Vesta
中文
源代码

KORTESTW, KORTESTB, KORTESTQ, KORTESTD

OR 遮盖和设置旗帜

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
VEX.L0.0F.W0 98 /rKORTESTW k1, k2RR有效有效位元 OR 16 比特 遮盖 k1 和 k2 ,并相应更新 ZF 和 CF. OR AVX10.1
VEX.L0.66.0F.W0 98 /rKORTESTB k1, k2RR有效有效位元 OR 8 比特遮盖 k1 和 k2 并相应更新 ZF 和 CF. OR AVX10.1
VEX.L0.0F.W1 98 /rKORTESTQ k1, k2RR有效有效位元 OR 64 位元口罩 k1 和 k2 并相应更新 ZF 和 CF. OR AVX10.1
VEX.L0.66.0F.W1 98 /rKORTESTD k1, k2RR有效有效位元 OR 32 位元口罩 k1 和 k2 并相应更新 ZF 和 CF. OR AVX10.1

操作数编码

每个模式对应上表 Op/En 列的一个取值，说明各操作数按书写顺序分别编码在指令的哪个字段，以及指令对它是读、是写还是两者兼有。

RR

  1. modrm.reg escrituraModRM 字节的 reg 字段（第 5-3 位）
  2. modrm.rm lecturaModRM 字节的 r/m 字段（第 2-0 位）；当 mod 字段要求时，还包括 SIB 字节和位移

实测开销

正在从 arch-data 加载实测数据...

涉及的标志位

说明

在矢量掩码登记k2和矢量掩码登记k1之间执行位元OR,并根据操作结果设置CF和ZF.

如果两个来源均为0x0,则设置ZF旗. 如果在OR操作完成后,操作结果为全部1's,则CF被设定.

行动

KORTESTW
TMP[15:0] := DEST[15:0] BITWISE OR SRC[15:0]
IF(TMP[15:0]=0)

    THEN ZF := 1
    ELSE ZF := 0
FI;
IF(TMP[15:0]=FFFFh)
    THEN CF := 1
    ELSE CF := 0
FI;

KORTESTB
TMP[7:0] := DEST[7:0] BITWISE OR SRC[7:0]
IF(TMP[7:0]=0)

    THEN ZF := 1
    ELSE ZF := 0
FI;
IF(TMP[7:0]==FFh)
    THEN CF := 1
    ELSE CF := 0

FI;


KORTESTQ
TMP[63:0] := DEST[63:0] BITWISE OR SRC[63:0]
IF(TMP[63:0]=0)

    THEN ZF := 1
    ELSE ZF := 0
FI;
IF(TMP[63:0]==FFFFFFFF_FFFFFFFFh)
    THEN CF := 1
    ELSE CF := 0
FI;

KORTESTD
TMP[31:0] := DEST[31:0] BITWISE OR SRC[31:0]
IF(TMP[31:0]=0)

    THEN ZF := 1
    ELSE ZF := 0
FI;
IF(TMP[31:0]=FFFFFFFFh)
    THEN CF := 1
    ELSE CF := 0
FI;

Intel C/C++ 内在编译器

KORTESTW __mmask16 _mm512_kortest[cz](__mmask16 a, __mmask16 b);

受影响的旗帜

如果两个源的OR-ing结果均为0s,则设置ZF旗.

如果两个源的OR-ing结果均为1s,则设定了CF旗.

OF, SF, AF,和PF的旗帜被设定为0.

其他例外

参见表2-65"TYPE K20例外定义(VEX-Encoded Opmask Directions w/o Memory Arg)".

来源