Vesta
Español
Código fuente

MOVNTPS

Tienda valores en coma flotante de precisión simple empaquetados Usando Hinte no Temporal

estableVMJITAOTinstruccion

Codificaciones

OpcodeInstruccionOp/En64 bitsCompat/LegacyDescripcion
NP 0F 2B /rMOVNTPS m128, xmm1AValidoValidoMover los valores de precisión simples empaquetados xmm1 a mem usando la indirecta no temporal.
VEX.128.0F.WIG 2B /rVMOVNTPS m128, xmm1AValidoValidoMover los valores de precisión simples empaquetados xmm1 a mem usando la indirecta no temporal.
VEX.256.0F.WIG 2B /rVMOVNTPS m256, ymm1AValidoValidoMover los valores de precisión simples empaquetados ymm1 a mem usando la indirecta no temporal.
EVEX.128.0F.W0 2B /rVMOVNTPS m128, xmm1BValidoValidoMover los valores de precisión simples empaquetados en xmm1 a m128 AVX512F) OR AVX10.1 usando la indirecta no temporal.
EVEX.256.0F.W0 2B /rVMOVNTPS m256, ymm1BValidoValidoMover los valores de precisión simples empaquetados en ymm1 a m256 AVX512F) OR AVX10.1 usando la indirecta no temporal.
EVEX.512.0F.W0 2B /rVMOVNTPS m512, zmm1 Op/En Tuple Type A N/A B Full MemBValidoValidoMover los valores de precisión simples en zmm1 a m512 Instru OR AVX10.1 ction operando Encoding1 utilizando indicios no temporales. O perand 1 operando 2 operando 3 operando 4 ModRM: r/m (w) ModRM:reg (r) N/A N/A

Codificacion de operandos

Cada modo es un valor de la columna Op/En de arriba. Dice en que campo de la instruccion codificada va cada operando, en el orden en que se escriben, y si la instruccion lo lee, lo escribe o ambas cosas.

A

  1. modrm.rm escriturabyte ModRM, campo r/m (bits 2-0); con el byte SIB y el desplazamiento cuando el campo mod los pide
  2. modrm.reg lecturabyte ModRM, campo reg (bits 5-3)

B

  1. modrm.rm escriturabyte ModRM, campo r/m (bits 2-0); con el byte SIB y el desplazamiento cuando el campo mod los pide
  2. modrm.reg lecturabyte ModRM, campo reg (bits 5-3)

Tupla: Full Mem

Coste medido

Cargando las mediciones de arch-data...

Descripción

Mueva los valores en coma flotante de precisión simple empaquetados en el operando de origen (segundo operando) al operando de destino (primer operando) utilizando una pista no temporal para evitar el caché de los datos durante el escrito a la memoria. El operando de origen es un registro XMM, registro YMM o registro ZMM, que se supone que contiene una sola precisión empaquetada, punto flotante. El operando de destino es una ubicación de memoria de 128 bits, 256 bits o 512 bits. El operando de memoria debe estar alineado en una versión de 16 bytes (128-bit), 32-byte (VEX.256 versión codificada) o 64-byte (EVEX.512 versión codificada) de lo contrario una excepción de protección general (#GP) se generará.

El indicio no temporal se implementa utilizando un protocolo de tipo de memoria de combinación de escritura (WC) al escribir los datos a la memoria. Utilizando este protocolo, el procesador no escribe los datos en la jerarquía de caché, ni recoge la línea correspondiente de caché de la memoria en la jerarquía de caché. El tipo de memoria de la región que se está escribiendo puede anular la indirecta no temporal, si la dirección de memoria especificada para la tienda no temporal está en una región de memoria inestable (UC) o escrita protegida (WP). Para obtener más información sobre las tiendas no temporales, consulte "Caching of Temporal vs. Datos no temporales" en el capítulo 10 del Manual de Desarrolladores de Software de Arquitectura Intel, Volumen 1.

Debido a que el protocolo WC utiliza un modelo de consistencia de memoria de orden débil, una operación de esgrima implementada con la instrucción SFENCE o MFENCE debe usarse junto con instrucciones MOVNTPS si varios procesadores pueden usar diferentes tipos de memoria para leer/escribir los lugares de memoria de destino.

Nota: VEX.vvvv y EVEX.vvvv están reservados y deben ser 1111b instrucciones de lo contrario #UD.

Operación

VMOVNTPS (EVEX Encoded Versions)
VL = 128, 256, 512
DEST[VL-1:0] := SRC[VL-1:0]
DEST[MAXVL-1:VL] := 0

1. ModRM.MOD != 011B


MOVNTPS
DEST := SRC

Intel C/C++ compilador intrínseco

VMOVNTPS void _mm512_stream_ps(float * p, __m512d a);
MOVNTPS void _mm_stream_ps (float * p, __m128d a);
VMOVNTPS void _mm256_stream_ps (float * p, __m256 a);

SIMD coma flotante Excepciones

None.

Otras excepciones

Instrucciones no-EVEX-encoded, ver Excepciones Tipo1.SSE en la tabla 2-18, "Tipo 1 Clase Condiciones de Excepción."

Instrucciones codificadas por EVEX, ver Tabla 2-47, "Tipo E1NF Clase Condiciones de Excepción."

Additionally:

#UD               If VEX.vvvv != 1111B or EVEX.vvvv != 1111B.

Fuentes