LDDQU
装入未对齐的128位元
stableVMJITAOTinstruction
编码
| 操作码 | 指令 | Op/En | 64 位 | 兼容/传统 | 说明 |
|---|---|---|---|---|---|
F2 0F F0 /r | LDDQU xmm1, mem | RM | 有效 | 有效 | 从 mem 装入不匹配的数据,并在 xmm1 中返回双四字 。 |
VEX.128.F2.0F.WIG F0 /r | VLDDQU xmm1, m128 | RM | 有效 | 有效 | 从 mem 装入不匹配的组合整数到 xmm1 。 |
VEX.256.F2.0F.WIG F0 /r | VLDDQU ymm1, m256 | RM | 有效 | 有效 | 从 mem 装入不匹配的组合整数到 ymm1 。 |
操作数编码
每个模式对应上表 Op/En 列的一个取值，说明各操作数按书写顺序分别编码在指令的哪个字段，以及指令对它是读、是写还是两者兼有。
RM
modrm.regescrituraModRM 字节的 reg 字段（第 5-3 位）modrm.rmlecturaModRM 字节的 r/m 字段（第 2-0 位）；当 mod 字段要求时，还包括 SIB 字节和位移
实测开销
正在从 arch-data 加载实测数据...
说明
该指令在功能上类似于(V)MOVDQU ymm/xmm,m256/m128从内存加载. 即:32/16字节数据从来源指定的地址内存操作数(第二位操作数)开始,从内存中获取,放入目的地登记册(第一位操作数). 源操作数不需要在32/16字节边界上对齐. 最多 64/ 32 字节可以从内存中装入; 这取决于执行 。
如果 源操作数 跨越缓存线边界,此指令可能会比 (V) MOVDQU 提高性能. 在需要(V)LDDQU加载的数据被修改并存储到同一位置的情况下,使用(V)MOVDQU或(V)MOVDQA代替(V)LDDQU. 要将双四字移动到已知16字节边界对齐的内存位置,请使用(V)MOVDQA指令.
执行说明
- 如果来源与32/16字节的边界一致,则基于执行,32/16字节可能是
装了不止一次 因此,在使用无标记或书写组合(WC)内存区域时,应避免使用(V)LDDQU. 对于未标记或WC内存区域,继续使用(V)MOVDQU.
- 此指令是在缓存行分割显著影响的情况下, (V) MOVDQU (载) 的替换
表现。 不应在储存量转发对性能至关重要的情况下使用。 如果存储负载转发的性能对应用程序至关重要,在数据为256/128位对齐时使用(V)MOVDQA存储负载对,在数据为256/128位不对齐时使用(V)MOVDQU存储负载对.
- 如果内存地址没有在32/16字节边界上对齐,一些执行可能会加载到64/32
字节并返回目的地的32/16字节. 一些处理器执行可能会发出多个负载来访问适当的32/16字节. 多线程或多处理器软件的开发者应当意识到,在这些处理器上,负载将以非原子方式完成.
- 如果启用对齐检查(CR0.AM = 1, RFLAGS.AC = 1, CPL = 3),则对齐检查例外
(#AC) 当内存地址没有在8字节边界上对齐时,可能生成也可能不会生成(取决于处理器执行).
在64位模式中,使用REX.R前缀允许此指令访问额外的注册(XMM8-XMM15).
说明: 在VEX-encoded版本中,VEX.vvvv被保留,必须是1111b否则指令会#UD.
行动
LDDQU (128-bit Legacy SSE Version)
DEST[127:0] := SRC[127:0]
DEST[MAXVL-1:128] (Unmodified)
VLDDQU (VEX.128 Encoded Version)
DEST[127:0] := SRC[127:0]
DEST[MAXVL-1:128] := 0
VLDDQU (VEX.256 Encoded Version)
DEST[255:0] := SRC[255:0]
DEST[MAXVL-1:256] := 0Intel C/C++ 内在编译器
LDDQU __m128i _mm_lddqu_si128 (__m128i * p);
VLDDQU __m256i _mm256_lddqu_si256 (__m256i * p);数字例外
None.
其他例外
参见表2-21"第4类例外条件",#AC的注解处理不尽相同.