Vesta
中文
源代码

AESDEC

执行 AES 解密流程的一回合

stableVMJITAOTinstruction

编码

操作码指令Op/En64 位兼容/传统说明
66 0F 38 DE /rAESDEC xmm1, xmm2/m128A有效有效执行AES解密流的一回合,使用等效反向密码,使用来自xmm1的128位数据(状态),使用来自xmm2/m128的128位圆密钥.
VEX.128.66.0F38.WIG DE /rVAESDEC xmm1, xmm2, xmm3/m128B有效有效执行AES解密流的一回合,使用AVX的等效反向密码,使用xmm2的一个128位数据(状态),使用xmm3/m128的一个128位圆的密钥;将结果存储在xmm1中.
VEX.256.66.0F38.WIG DE /rVAESDEC ymm1, ymm2, ymm3/m256B有效有效执行AES解密流的一回合,使用等效反向密码,使用ymm2的两个128位数据(状态),用ymm3/m256的两个128位圆的密钥;将结果存储在ymm1中.
EVEX.128.66.0F38.WIG DE /rVAESDEC xmm1, xmm2, xmm3/m128C有效有效执行一回合AES解密流,使用(AVX512VL OR AVX10.1)等效反向密码器,使用xmm2的128位数据(状态),使用xmm3/m128的128位圆键;将结果存储为xmm1.
EVEX.256.66.0F38.WIG DE /rVAESDEC ymm1, ymm2, ymm3/m256C有效有效进行一回合的比赛AES解密流量,使用(AVX512VL或AVX10.1) 等效反向密码,使用两个128位数据(状态)从ymm2带有两个 128 位圆密钥从ymm3/m256; 将结果存储到ymm1.
EVEX.512.66.0F38.WIG DE /rVAESDEC zmm1, zmm2, zmm3/m512C有效有效进行一回合的比赛AES解密流量,使用(AVX512F或AVX10.1) 等效反向密码,使用四个128位数据(状态)从zmm24个128位圆密钥从zmm3/m512; 将结果存储到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位数据(状态)与来自第二源操作数的密钥(矢量长度)圆,并存储结果为目标操作数.

使用 AESDEC 指令除最后一个解密回合外的所有对象。 对于最后一个解密回合,使用AESDE-CLAST指令.

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

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

行动

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

VAESDEC (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 )
    STATE := InvMixColumns( STATE )
    DEST.xmm[i] := STATE XOR RoundKey
DEST[MAXVL-1:VL] := 0

VAESDEC (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 )
    STATE := InvMixColumns( STATE )
    DEST.xmm[i] := STATE XOR RoundKey
DEST[MAXVL-1:VL] :=0

Intel C/C++ 内在编译器

(V)AESDEC __m128i _mm_aesdec (__m128i, __m128i) VAESDEC __m256i _mm256_aesdec_epi128(__m256i, __m256i);
VAESDEC __m512i _mm512_aesdec_epi128(__m512i, __m512i);

SIMD 浮点 例外

None.

其他例外

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

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

来源