Vesta
Español
Código fuente

VPERMT2B

Full Permute of Bytes De Dos Tablas Sobreescribir una Tabla

estableVMJITAOTinstruccion

Codificaciones

OpcodeInstruccionOp/En64 bitsCompat/LegacyDescripcion
EVEX.128.66.0F38.W0 7D /rVPERMT2B xmm1 {k1}{z}, xmm2, xmm3/m128AValidoValidoPermute bytes en xmm3/m128 y xmm1 usando AVX512 VBMI) índices de byte en xmm2 y almacenar los resultados de byte en OR AVX10.1 xmm1 utilizando máscara de escritura k1.
EVEX.256.66.0F38.W0 7D /rVPERMT2B ymm1 {k1}{z}, ymm2, ymm3/m256AValidoValidoPermute bytes en ymm3/m256 y ymm1 usando AVX512 VBMI) índices de byte en ymm2 y almacenar los resultados de byte en OR AVX10.1 ymm1 utilizando máscara de escritura k1.
EVEX.512.66.0F38.W0 7D /rVPERMT2B zmm1 {k1}{z}, zmm2, zmm3/m512AValidoValidoPermute bytes en zmm3/m512 y zmm1 usando índices de byte OR AVX10.1 en zmm2 y almacenar los resultados de byte en zmm1 utilizando scriptmask k1.

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.reg lectura y escriturabyte ModRM, campo reg (bits 5-3)
  2. evex.vvvv lecturaprefijo EVEX, campo vvvv (invertido)
  3. modrm.rm lecturabyte ModRM, campo r/m (bits 2-0); con el byte SIB y el desplazamiento cuando el campo mod los pide

Tupla: Full Mem

Coste medido

Cargando las mediciones de arch-data...

Descripción

Permutes byte values from two tables, comprising of the first operand (also the destination operand) and the third operand (the second source operand). El segundo operando (el primer operando de origen) proporciona índices de byte para seleccionar los resultados de byte de las dos tablas. Los elementos de byte seleccionados se escriben al destino a byte granularity bajo la máscara de escritura k1.

El primero y segundo operandos son los registros ZMM/YMM/XMM. El segundo operando contiene índices de entrada para seleccionar elementos de las dos tablas de entrada en el primer y tercer operandos. El primer operando es también el destino del resultado. El segundo operando de origen puede ser un registro ZMM/YMM/XMM, o un 512/256/128-bit ubicación de memoria. En cada byte índice, el bit id para la selección de tablas es bit 6/5/4, y bits [5:0]/[4:0]/[3:0] selecciona el elemento dentro de cada tabla de entrada.

Tenga en cuenta que estas instrucciones permiten copiar un valor byte en los operandos de origen a más de un lugar en el operando de destino. Además, la segunda tabla y los índices se pueden reutilizar en las iteraciones posteriores, pero la primera tabla está sobrescrito.

Bits (MAX VL-1:256/128) del destino se ponen a cero para VL=256,128.

Operación

VPERMT2B (EVEX encoded versions)
(KL, VL) = (16, 128), (32, 256), (64, 512)
IF VL = 128:

    id := 3;
ELSE IF VL = 256:

    id := 4;
ELSE IF VL = 512:

    id := 5;
FI;
TMP_DEST[VL-1:0] := DEST[VL-1:0];
FOR j := 0 TO KL-1

    off := 8*SRC1[j*8 + id: j*8] ;
    IF k1[j] OR *no writemask*:

          DEST[j*8 + 7: j*8] := SRC1[j*8+id+1]? SRC2[off+7:off] : TMP_DEST[off+7:off];
    ELSE IF *zeroing-masking*

          DEST[j*8 + 7: j*8] := 0;
    *ELSE

          DEST[j*8 + 7: j*8] remains unchanged*
    FI;
ENDFOR
DEST[MAX_VL-1:VL] := 0;

Intel C/C++ compilador intrínseco

VPERMT2B __m512i _mm512_permutex2var_epi8(__m512i a, __m512i idx, __m512i b);
VPERMT2B __m512i _mm512_mask_permutex2var_epi8(__m512i a, __mmask64 k, __m512i idx, __m512i b);
VPERMT2B __m512i _mm512_maskz_permutex2var_epi8(__mmask64 k, __m512i a, __m512i idx, __m512i b);
VPERMT2B __m256i _mm256_permutex2var_epi8(__m256i a, __m256i idx, __m256i b);
VPERMT2B __m256i _mm256_mask_permutex2var_epi8(__m256i a, __mmask32 k, __m256i idx, __m256i b);
VPERMT2B __m256i _mm256_maskz_permutex2var_epi8(__mmask32 k, __m256i a, __m256i idx, __m256i b);
VPERMT2B __m128i _mm_permutex2var_epi8(__m128i a, __m128i idx, __m128i b);
VPERMT2B __m128i _mm_mask_permutex2var_epi8(__m128i a, __mmask16 k, __m128i idx, __m128i b);
VPERMT2B __m128i _mm_maskz_permutex2var_epi8(__mmask16 k, __m128i a, __m128i idx, __m128i b);

SIMD coma flotante Excepciones

None.

Otras excepciones

Ver Excepciones Tipo E4NF.nb en la tabla 2-52, "Tipo E4NF Clase Condiciones de Excepción."

Fuentes