KNOTW, KNOTB, KNOTQ, KNOTD

NOT Mask Register

estableVMJITAOTinstruccion

Codificaciones

OpcodeInstruccionOp/En64 bitsCompat/LegacyDescripcion
VEX.L0.0F.W0 44 /rKNOTW k1, k2RRValidoValidoBitwise NOT de 16 bits máscara k2. OR AVX10.1
VEX.L0.66.0F.W0 44 /rKNOTB k1, k2RRValidoValidoBitwise NOT de 8 bits máscara k2. OR AVX10.1
VEX.L0.0F.W1 44 /rKNOTQ k1, k2RRValidoValidoBitwise NOT de 64 bits máscara k2. OR AVX10.1
VEX.L0.66.0F.W1 44 /rKNOTD k1, k2RRValidoValidoBitwise NOT de 32 bits máscara k2. OR AVX10.1

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.

RR

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

Coste medido

Cargando las mediciones de arch-data...

Descripción

Realiza un bitwise NOT de máscara vectorial k2 y escribe el resultado en máscara vectorial k1.

Operación

KNOTW
DEST[15:0] := BITWISE NOT SRC[15:0]
DEST[MAX_KL-1:16] := 0

KNOTB
DEST[7:0] := BITWISE NOT SRC[7:0]
DEST[MAX_KL-1:8] := 0

KNOTQ
DEST[63:0] := BITWISE NOT SRC[63:0]
DEST[MAX_KL-1:64] := 0

KNOTD
DEST[31:0] := BITWISE NOT SRC[31:0]
DEST[MAX_KL-1:32] := 0

Intel C/C++ compilador intrínseco

KNOTW __mmask16 _mm512_knot(__mmask16 a);

Banderas afectadas

None.

SIMD coma flotante Excepciones

None.

Otras excepciones

Ver Tabla 2-65, "TYPE K20 Excepción Definición (VEX-Encoded OpMask Instrucciones w/o Memoria Arg)."

Fuentes