Vesta
中文
源代码

AESDECLAST

执行 AES 解密流程的最后一轮

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
66 0F 38 DF /rAESDECLAST xmm1, xmm2/m128A有效有效执行 AES 解密流的最后一回合,使用等效反向密码,使用来自 xmm1 的 1 128位数据(状态),使用来自 xmm2/m128 的 1 128位圆 密钥 .
VEX.128.66.0F38.WIG DF /rVAESDECLAST xmm1, xmm2, xmm3/m128B有效有效执行 AES 解密流的最后一回合,AVX 使用等效反向密码,使用 xmm2 的 1 128位数据(状态),使用 xmm3/m128 的 1 128位圆键;将结果存储在 xmm1 中.
VEX.256.66.0F38.WIG DF /rVAESDECLAST ymm1, ymm2, ymm3/m256B有效有效执行 AES 解密流的最后一回合,使用等效反向密码,使用 ymm2 的两个128位数据(状态),用 ymm3/m256 的两个128位圆的 密钥;将结果存储在 ymm1 中.
EVEX.128.66.0F38.WIG DF /rVAESDECLAST xmm1, xmm2, xmm3/m128C有效有效使用等效反向密码器执行 AES 解密流的最后一回合(AVX512VL OR AVX10.1),使用 xmm2 的 1 128位数据(状态),并使用 xmm3/m128 的 1 128位圆键;将结果存储在 xmm1 中.
EVEX.256.66.0F38.WIG DF /rVAESDECLAST ymm1, ymm2, ymm3/m256C有效有效使用等效反向密码器执行AES解密流的最后一回合(AVX512VL OR AVX10.1),使用ymm2的2个128位数据(状态),用ymm3/m256的2个128位圆密钥;将结果存储为ymm1.
EVEX.512.66.0F38.WIG DF /rVAESDECLAST zmm1, zmm2, zmm3/m512C有效有效使用等效反向密码器执行AES解密流的最后一回合(AVX512F OR AVX10.1),使用zmm2的4128位数据(状态),用zmm3/m512的4个128位圆的密钥;将结果存储在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 加载实测数据...

说明

本指令使用等效反向塞弗进行AES解密流的最后一回合,使用来自第一源操作数的128位数据(状态)与来自第二源操作数的密钥(矢量长度)圆,并存储结果为目标操作数.

VEX和EVEX编码的指令版本允许3-操作数(无损)操作. 指令的遗留编码版本要求第一源操作数和目标操作数是相同的,必须是一个XMM的登记册.

本指令的EVEX编码形式不支持内存断层压制.

行动

AESDECLAST
STATE := SRC1;
RoundKey := SRC2;
STATE := InvShiftRows( STATE );
STATE := InvSubBytes( STATE );
DEST[127:0] := STATE XOR RoundKey;
DEST[MAXVL-1:128] (Unmodified)

VAESDECLAST (128b and 256b VEX Encoded Versions)
(KL,VL) = (1,128), (2,256)
FOR i = 0 to KL-1:

    STATE := SRC1.xmm[i]
    RoundKey := SRC2.xmm[i]
    STATE := InvShiftRows( STATE )
    STATE := InvSubBytes( STATE )
    DEST.xmm[i] := STATE XOR RoundKey
DEST[MAXVL-1:VL] := 0

VAESDECLAST (EVEX Encoded Version)
(KL,VL) = (1,128), (2,256), (4,512)
FOR i = 0 to KL-1:

    STATE := SRC1.xmm[i]
    RoundKey := SRC2.xmm[i]
    STATE := InvShiftRows( STATE )
    STATE := InvSubBytes( STATE )
    DEST.xmm[i] := STATE XOR RoundKey
DEST[MAXVL-1:VL] := 0

Intel C/C++ 内在编译器

(V)AESDECLAST __m128i _mm_aesdeclast (__m128i, __m128i) VAESDECLAST __m256i _mm256_aesdeclast_epi128(__m256i, __m256i);
VAESDECLAST __m512i _mm512_aesdeclast_epi128(__m512i, __m512i);

SIMD 浮点 例外

None.

其他例外

参见表2-21"第4类例外条件".

EVEX 编码 : 参见表2-52"Type E4NF类例外条件".

来源