Vesta
中文
源代码

PSUBSB, PSUBSW

带有签名饱和度的 有符号整数 包装的减法

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
NP 0F E8 /r1PSUBSB mm, mm/m64A有效有效以毫米/m64为单位,从以毫米和饱和结果为单位的已签名的已包装字节中减除。
66 0F E8 /rPSUBSB xmm1, xmm2/m128A有效有效从xmm1和饱和结果的已包装的已签名字节整数中减去xmm2/m128的已签名字节整数。
NP 0F E9 /r1PSUBSW mm, mm/m64A有效有效以毫米/m64为单位,从以毫米和饱和结果为单位的签名的包装单词中减去已签名的包装单词。
66 0F E9 /rPSUBSW xmm1, xmm2/m128A有效有效从xmm1和饱和结果中的已打包的已签单词整数中减去xmm2/m128中的已签单词整数。
VEX.128.66.0F.WIG E8 /rVPSUBSB xmm1, xmm2, xmm3/m128B有效有效从xmm2和饱和结果的已包装的已签名字节整数中减去xmm3/m128的已签名字节整数。
VEX.128.66.0F.WIG E9 /rVPSUBSW xmm1, xmm2, xmm3/m128B有效有效从xmm2和饱和结果中的已打包的已签单词整数中减去xmm3/m128中的已签单词整数。
VEX.256.66.0F.WIG E8 /rVPSUBSB ymm1, ymm2, ymm3/m256B有效有效从ymm2和饱和结果的已包装的已签名字节整数中减去ymm3/m256的已签名字节整数。
VEX.256.66.0F.WIG E9 /rVPSUBSW ymm1, ymm2, ymm3/m256B有效有效从ymm2和饱和结果中的已打包的已签单词整数中减去ymm3/m256中的已签单词整数。
EVEX.128.66.0F.WIG E8 /rVPSUBSB xmm1 {k1}{z}, xmm2, xmm3/m128C有效有效从AVX10.1 xmm2的已包装字节整数和饱和结果中减去xmm1的已签名字节整数(AVX512BW)或xmm3/m128,并使用writemask k1在xmm1中存储.
EVEX.256.66.0F.WIG E8 /rVPSUBSB ymm1 {k1}{z}, ymm2, ymm3/m256C有效有效从AVX10.1 ymm2的已包装字节整数和饱和结果中减去ymm1的已签名字节整数(AVX512BW)或ymm3/m256,并使用writemask k1在ymm1中存储.
EVEX.512.66.0F.WIG E8 /rVPSUBSB zmm1 {k1}{z}, zmm2, zmm3/m512C有效有效在OR AVX10.1 zmm3/m512中,从zmm2中和饱和结果中分别将已签名的字节整数和用写掩码 k1在zmm1中存储.
EVEX.128.66.0F.WIG E9 /rVPSUBSW xmm1 {k1}{z}, xmm2, xmm3/m128C有效有效从AVX10.1 xmm2的已包装的已签名单词整数和饱和结果中减去xmm1的已签名单词整数(AVX512BW)OR xmm3/m128,并使用写掩码 k1存储在xmm1.
EVEX.256.66.0F.WIG E9 /rVPSUBSW ymm1 {k1}{z}, ymm2, ymm3/m256C有效有效从AVX10.1 ymm2的已包装的已签名单词整数和饱和结果中减去ymm1的已签名单词整数(AVX512BW)OR ymm3/m256,并使用写掩码 k1存储在ymm1.
EVEX.512.66.0F.WIG E9 /rVPSUBSW zmm1 {k1}{z}, zmm2, zmm3/m512C有效有效在OR AVX10.1 zmm3/m512中,从zmm2中和饱和结果中分别将已包装的已签名单词整数和用写掩码 k1存储在zmm1中.

操作数编码

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

A

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

B

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

C

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

Tupla: Full Mem

实测开销

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

说明

执行 SIMD 从目标操作器的已包装签名整数中减去来源操作器的已包装签名整数(第二个操作器),并将已包装的整数结果存储在目的操作器中。 参见Intel(R)64和IA-32 Architectures Software开发者手册第1卷图9-4中的SIMD操作的插图. 如以下各段所述,通过签名饱和处理过度流量。

(V) PSUBSB 指令减去了所包装的签名字节整数。 当单个字节结果超出一个签名字节整数的范围(即大于7FH或小于80H)时,7FH或80H的饱和值分别写成目标操作数.

(V) PSUBSW 指令减去已打包的签名单词整数。 当单个单词结果超过签名单词整数的范围(即大于7FFFH或小于8000H)时,7FFFH或8000H的饱和值分别写成目标操作数.

在64位模式中,没有用VEX/EVEX编码,使用REX前缀形式为REX.R允许此指令访问额外的注册(XMM8-XMM15).

遗产 SSE版本 64位 操作数: 目标操作数必须是MMX技术登记册,源操作数可以是MMX技术登记册,也可以是64位内存位置技术登记册.

128位遗产 SSE 版本 : 第二源操作数是一个XMM的寄存器或128位的内存位置. 第一源操作数和目标操作数是XMM登记册. 相应的YMM目的地注册保持不变的位数(MAXVL-1:128).

VEX.128 编码版本 : 第二源操作数是一个XMM的寄存器或128位的内存位置. 第一源操作数和目标操作数是XMM登记册. 目的地YMM的位数(MAXVL-1:128)登记被清零.

VEX.256 编码版本 : 第二源操作数是一个YMM的寄存器或256位的内存位置. 第一源操作数和目标操作数是YMM登记册. 对应的ZMM注册被清零的位数(MAXVL-1:256).

EVEX 编码版本 : 第二源操作数是一个ZMM/YMM/XMM的登记册或512/256/128位内存位置. 第一源操作数和目标操作数是ZMM/YMM/XMM登记册. 目的地以写掩码 k1有条件更新.

行动

PSUBSB (With 64-bit Operands)
    DEST[7:0] := SaturateToSignedByte (DEST[7:0] - SRC (7:0]);
    (* Repeat subtract operation for 2nd through 7th bytes *)
    DEST[63:56] := SaturateToSignedByte (DEST[63:56] - SRC[63:56] );


PSUBSW (With 64-bit Operands)
    DEST[15:0] := SaturateToSignedWord (DEST[15:0] - SRC[15:0] );
    (* Repeat subtract operation for 2nd and 7th words *)
    DEST[63:48] := SaturateToSignedWord (DEST[63:48] - SRC[63:48] );

VPSUBSB (EVEX Encoded Versions)

(KL, VL) = (16, 128), (32, 256), (64, 512)

FOR j := 0 TO KL-1

i := j * 8;

IF k1[j] OR *no writemask*

     THEN DEST[i+7:i] := SaturateToSignedByte (SRC1[i+7:i] - SRC2[i+7:i])

     ELSE

             IF *merging-masking*           ; merging-masking

                 THEN *DEST[i+7:i] remains unchanged*

                 ELSE *zeroing-masking*     ; zeroing-masking

                    DEST[i+7:i] := 0;

             FI

FI;

ENDFOR;

DEST[MAXVL-1:VL] := 0

VPSUBSW (EVEX Encoded Versions)

(KL, VL) = (8, 128), (16, 256), (32, 512)

FOR j := 0 TO KL-1

i := j * 16

IF k1[j] OR *no writemask*

     THEN DEST[i+15:i] := SaturateToSignedWord (SRC1[i+15:i] - SRC2[i+15:i])

     ELSE

             IF *merging-masking*           ; merging-masking

                 THEN *DEST[i+15:i] remains unchanged*

                 ELSE *zeroing-masking*     ; zeroing-masking

                    DEST[i+15:i] := 0;

             FI

FI;

ENDFOR;

DEST[MAXVL-1:VL] := 0;

VPSUBSB (VEX.256 Encoded Version)
DEST[7:0] := SaturateToSignedByte (SRC1[7:0] - SRC2[7:0]);
(* Repeat subtract operation for 2nd through 31th bytes *)
DEST[255:248] := SaturateToSignedByte (SRC1[255:248] - SRC2[255:248]);
DEST[MAXVL-1:256] := 0;

VPSUBSB (VEX.128 Encoded Version)
DEST[7:0] := SaturateToSignedByte (SRC1[7:0] - SRC2[7:0]);
(* Repeat subtract operation for 2nd through 14th bytes *)
DEST[127:120] := SaturateToSignedByte (SRC1[127:120] - SRC2[127:120]);
DEST[MAXVL-1:128] := 0;

PSUBSB (128-bit Legacy SSE Version)
DEST[7:0] := SaturateToSignedByte (DEST[7:0] - SRC[7:0]);
(* Repeat subtract operation for 2nd through 14th bytes *)
DEST[127:120] := SaturateToSignedByte (DEST[127:120] - SRC[127:120]);
DEST[MAXVL-1:128] (Unmodified);


VPSUBSW (VEX.256 Encoded Version)
DEST[15:0] := SaturateToSignedWord (SRC1[15:0] - SRC2[15:0]);
(* Repeat subtract operation for 2nd through 15th words *)
DEST[255:240] := SaturateToSignedWord (SRC1[255:240] - SRC2[255:240]);
DEST[MAXVL-1:256] := 0;

VPSUBSW (VEX.128 Encoded Version)
DEST[15:0] := SaturateToSignedWord (SRC1[15:0] - SRC2[15:0]);
(* Repeat subtract operation for 2nd through 7th words *)
DEST[127:112] := SaturateToSignedWord (SRC1[127:112] - SRC2[127:112]);
DEST[MAXVL-1:128] := 0;

PSUBSW (128-bit Legacy SSE Version)
DEST[15:0] := SaturateToSignedWord (DEST[15:0] - SRC[15:0]);
(* Repeat subtract operation for 2nd through 7th words *)
DEST[127:112] := SaturateToSignedWord (DEST[127:112] - SRC[127:112]);
DEST[MAXVL-1:128] (Unmodified);

Intel C/C++ 内在编译器

VPSUBSB __m512i _mm512_subs_epi8(__m512i a, __m512i b);
VPSUBSB __m512i _mm512_mask_subs_epi8(__m512i s, __mmask64 k, __m512i a, __m512i b);
VPSUBSB __m512i _mm512_maskz_subs_epi8( __mmask64 k, __m512i a, __m512i b);
VPSUBSB __m256i _mm256_mask_subs_epi8(__m256i s, __mmask32 k, __m256i a, __m256i b);
VPSUBSB __m256i _mm256_maskz_subs_epi8( __mmask32 k, __m256i a, __m256i b);
VPSUBSB __m128i _mm_mask_subs_epi8(__m128i s, __mmask16 k, __m128i a, __m128i b);
VPSUBSB __m128i _mm_maskz_subs_epi8( __mmask16 k, __m128i a, __m128i b);
VPSUBSW __m512i _mm512_subs_epi16(__m512i a, __m512i b);
VPSUBSW __m512i _mm512_mask_subs_epi16(__m512i s, __mmask32 k, __m512i a, __m512i b);
VPSUBSW __m512i _mm512_maskz_subs_epi16( __mmask32 k, __m512i a, __m512i b);
VPSUBSW __m256i _mm256_mask_subs_epi16(__m256i s, __mmask16 k, __m256i a, __m256i b);
VPSUBSW __m256i _mm256_maskz_subs_epi16( __mmask16 k, __m256i a, __m256i b);
VPSUBSW __m128i _mm_mask_subs_epi16(__m128i s, __mmask8 k, __m128i a, __m128i b);
VPSUBSW __m128i _mm_maskz_subs_epi16( __mmask8 k, __m128i a, __m128i b);
PSUBSB __m64 _mm_subs_pi8(__m64 m1, __m64 m2) (V)PSUBSB __m128i _mm_subs_epi8(__m128i m1, __m128i m2) VPSUBSB __m256i _mm256_subs_epi8(__m256i m1, __m256i m2) PSUBSW __m64 _mm_subs_pi16(__m64 m1, __m64 m2) (V)PSUBSW __m128i _mm_subs_epi16(__m128i m1, __m128i m2) VPSUBSW __m256i _mm256_subs_epi16(__m256i m1, __m256i m2);

受影响的旗帜

None.

数字例外

None.

其他例外

Non-EVEX-encoded discription,参见表2-21"第4类例外条件".

EVEX-encoded 指令,参见表2-51中的例外类型E4.nb,"Type E4类例外条件".

来源