aarch64-gcc simd inline asm，结果始终为0

Question

我尝试使用Inline Assembler进行SIMD乘法。但是，结果始终为零，或者（在其他情况下）变得难以置信（对我来说）值。

#include <stdio.h>

int main(void)
{
        double x[2] = {2.0, 3.0};
        double y[2] = {0.0, 0.0};

        asm volatile (
              "fmul %[y].2d, %[x].2d, %[x].2d\n"
        : /* outputs */
          [y] "=&w" (y)
        : /* inputs */
          [x] "w" (x)
        : /* clobbers */
          "cc"
        );

        printf("result = (%f, %f)\n",
               y[0], y[1]);

        return 0;
}

我总是会收集

aarch64-linux-gnu-gcc -mcpu=cortex-a73 -march='armv8-a'

输出，

result = (0.000000, 0.000000)

但我希望（4.0，9.0）。请帮忙！

Answer 1

正如杰斯特所说，您必须将 value 传递给asm语句，而不是指向相关基准的指针。此值的正确类型是float64x2_t来自arm_neon.h。因此，请按以下方式进行：

#include <stdio.h>
#include <arm_neon.h>

int main(void)
{
        double x[2] = {2.0, 3.0};
        double y[2] = {0.0, 0.0};

        asm volatile (
              "fmul %[y].2d, %[x].2d, %[x].2d\n"
        : /* outputs */
          [y] "=&w" (*(float64x2_t *)y)
        : /* inputs */
          [x] "w" (*(float64x2_t *)x)
        : /* clobbers */
          "cc"
        );

        printf("result = (%f, %f)\n",
               y[0], y[1]);

        return 0;
}

请注意，当您包含内在标题时，您不妨直接使用内在信息：

int bar(void)
{
        double x[2] = {2.0, 3.0};
        double y[2] = {0.0, 0.0};
        float64x2_t *xx = x, *yy = y;

        *yy = vmulq_f64(*xx, *xx);

        printf("result = (%f, %f)\n",
               y[0], y[1]);

        return 0;
}