Vesta
中文
源代码

PMOVMSKB

移动字节遮罩 Op/ 64/ 32 位 CPUID

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
NP 0F D7 /r1PMOVMSKB reg, mmRM有效有效将一个毫米的字节掩码移动到正则。 r32 或 r64 被清零 的上位位
66 0F D7 /rPMOVMSKB reg, xmmRM有效有效将 xmm 的字节掩码移动到正则。 r32 或 r64 的上位是零
VEX.128.66.0F.WIG D7 /rVPMOVMSKB reg, xmm1RM有效有效将 xmm1 的字节掩码移动到 reg 。 r32 或 r64 的上位位被零填充 。
VEX.256.66.0F.WIG D7 /rVPMOVMSKB reg, ymm1RM有效有效将 ymm1 的 32 位掩码移到 reg 中, r64 的上位被零填充.

操作数编码

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

RM

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

实测开销

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

说明

创建由源操作数(第二操作数)每个字节中最显著位组成的遮罩,并存储结果为目标操作数(第一操作数)的低字节或单词.

字节口罩为8位为64位源操作数,16位为128位源操作数,32位为256位源操作数. 目标操作数是一个通用寄存器.

在64位模式下,指令可以访问额外的注册(XMM8-XMM15, R8-R15与 a 一起使用时REX.R前缀。 默认的操作数大小为64位,模式为64位.

遗产 SSE 版本 : 源操作数是一个MMX技术登记册.

128位遗产 SSE 版本 : 源操作数是一个XMM登记册.

VEX.128 编码版本 : 源操作数是一个XMM登记册.

VEX.256 编码版本 : 源操作数是一个YMM登记册.

说明: VEX.vvvv是保留的,必须是1111b.

行动

PMOVMSKB (With 64-bit Source Operand and r32)

    r32[0] := SRC[7];
    r32[1] := SRC[15];
    (* Repeat operation for bytes 2 through 6 *)
    r32[7] := SRC[63];
    r32[31:8] := ZERO_FILL;


(V)PMOVMSKB (With 128-bit Source Operand and r32)
    r32[0] := SRC[7];
    r32[1] := SRC[15];
    (* Repeat operation for bytes 2 through 14 *)
    r32[15] := SRC[127];
    r32[31:16] := ZERO_FILL;

VPMOVMSKB (With 256-bit Source Operand and r32)
r32[0] := SRC[7];
r32[1] := SRC[15];
(* Repeat operation for bytes 3rd through 31*)
r32[31] := SRC[255];

PMOVMSKB (With 64-bit Source Operand and r64)
    r64[0] := SRC[7];
    r64[1] := SRC[15];
    (* Repeat operation for bytes 2 through 6 *)
    r64[7] := SRC[63];
    r64[63:8] := ZERO_FILL;

(V)PMOVMSKB (With 128-bit Source Operand and r64)
    r64[0] := SRC[7];
    r64[1] := SRC[15];
    (* Repeat operation for bytes 2 through 14 *)
    r64[15] := SRC[127];
    r64[63:16] := ZERO_FILL;

VPMOVMSKB (With 256-bit Source Operand and r64)
r64[0] := SRC[7];
r64[1] := SRC[15];
(* Repeat operation for bytes 2 through 31*)
r64[31] := SRC[255];
r64[63:32] := ZERO_FILL;

Intel C/C++ 内在编译器

PMOVMSKB int _mm_movemask_pi8(__m64 a) (V)PMOVMSKB int _mm_movemask_epi8 ( __m128i a) VPMOVMSKB int _mm256_movemask_epi8 ( __m256i a);

受影响的旗帜

None.

数字例外

None.

其他例外

见表2-24,"第7类例外条件",另外:

#UD                 If VEX.vvvv  1111B.

来源