内联汇编代码来读/写 XMM 和 YMM 寄存器？

Question

我有 2 个变量来模拟 X86 XMM 和 YMM，如下所示：

uint64_t xmm_value[2];
uint64_t ymm_value[4];

现在我想使用内联汇编来读写 XMM/YMM 寄存器。

• 如何编写GCC内联汇编复制xmm_value到注册XMM0？
• 如何编写 GCC 内联汇编将寄存器YMM0 复制到ymm_value？

我已经尝试搜索执行此操作的示例内联汇编，但找不到任何好的答案。谢谢！

---

在一些帮助下，我编写了这段代码，并且编译成功。我对 XMM 使用 movups，对 YMM 使用 vmovups，如下所示。这是正确的，我还能优化我的代码吗？

__m128 xmm0;
__m256 ymm0;

// write to XMM0, and read from YMM0
__asm__("movups %1, %%xmm0\n\t"
        "vmovups %%ymm0, %0"
        : "=m"(ymm0)
        : "m"(xmm0)
        : "xmm0", "ymm0");

---

更新 2：这是我的完整代码（添加了 vpbroadcastb）

__m128 xmm0;
__m256 ymm0;

// write to XMM0, and read from YMM0
__asm__("movups %1, %%xmm0\n\t"
        "vpbroadcastb %%xmm0, %%ymm0\n\t"
        "vmovups %%ymm0, %0"
        : "=m"(ymm0)
        : "m"(xmm0)
        : "xmm0", "ymm0");

想法是我想将xmm0（变量）复制到XMM0，然后运行vpbroadcastb，然后将YMM0中的结果复制到ymm0（变量）。现在才知道XMM0是YMM0的下半部分，所以这段代码还可以改进吗？

Answer 1

第一步是#include <immintrin.h>，其中包括所需类型的所有定义以及用于访问所有 MMX/SSE/AVX 指令的所有Intel Intrinsics。在大多数情况下，您希望使用这些内在函数而不是内联汇编，因为它们更清晰、更便携，但如果您真的想使用内联 asm，您可以使用内在类型（__m64、__m128、@987654325 @、__m256 等）以及 x 约束以绑定到正确类型的 xmm/ymm 寄存器。