Vesta
中文
源代码

MOVMSKPS

提取包装的 单精度浮点 签名罩

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
NP 0F 50 /rMOVMSKPS reg, xmmRM有效有效从 xmm 中提取 4- 位符号掩码, 并存储在 reg 中。 r32 或 r64 的上位被零填充 。
VEX.128.0F.WIG 50 /rVMOVMSKPS reg, xmm2RM有效有效从 xmm2 中提取 4- 位符号掩码,并以 reg 存储。 r32 或 r64 的上位符号为零 。
VEX.256.0F.WIG 50 /rVMOVMSKPS reg, ymm2 Op/En Operand 1 RM ModRM:reg (w)RM有效有效从 ymm2 中提取 8 位符号掩码,并以 reg 存储. r32 或 r64 的上位符号 被清零. Instr puction 操作数 编码 1 O perand 2 操作数 3 操作数 4 ModRM :r/m (r) N/A N/A

操作数编码

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

RM

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

实测开销

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

说明

从 源操作数 (秒 操作数) 中的 打包单精度浮点值 中提取符号位,将其格式化为4位或8位的面具,并将面具存储在 目标操作数 (第一个操作数)中. 源操作数是一个XMM或YMM登记册,目标操作数是一个通用寄存器. 面具保存在目标操作数的4或8低序位. 目标操作数超过面具的上位位被零填充.

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

128位版本 : 源操作数是一个YMM登记册. 目标操作数是一个通用注册.

VEX.256 编码版本 : 源操作数是一个YMM登记册. 目标操作数是一个通用注册.

说明: 在VEX-encoded版本中,VEX.vvvv是保留的,必须是1111b,否则指令会#UD.

行动

DEST[0] := SRC[31];
DEST[1] := SRC[63];
DEST[2] := SRC[95];
DEST[3] := SRC[127];

IF DEST = r32
    THEN DEST[31:4] := ZeroExtend;
    ELSE DEST[63:4] := ZeroExtend;

FI;

1. ModRM.MOD = 011B required


(V)MOVMSKPS (128-bit version)
DEST[0] := SRC[31]
DEST[1] := SRC[63]
DEST[2] := SRC[95]
DEST[3] := SRC[127]
IF DEST = r32

    THEN DEST[31:4] := 0;
    ELSE DEST[63:4] := 0;
FI

VMOVMSKPS (VEX.256 encoded version)
DEST[0] := SRC[31]
DEST[1] := SRC[63]
DEST[2] := SRC[95]
DEST[3] := SRC[127]
DEST[4] := SRC[159]
DEST[5] := SRC[191]
DEST[6] := SRC[223]
DEST[7] := SRC[255]
IF DEST = r32

    THEN DEST[31:8] := 0;
    ELSE DEST[63:8] := 0;
FI

Intel C/C++ 内在编译器

int _mm_movemask_ps(__m128 a) int _mm256_movemask_ps(__m256 a);

SIMD 浮点 例外

None.

其他例外

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

#UD               If VEX.vvvv  1111B.

来源