交叉編譯支持SVE ACLE的gcc

最近在學習AArch64的SVE技術時，發現目前可以在網上找到的gcc版本都不支持SVE intrinsic方式調用，在看文檔時發現，GCC要到2020年的GCC10時才會支持：

 

 在github上看到了gcc倉庫里存在一個名為aarch64/sve-acle-branch的分支：

 

然后將這個分支的代碼下載下來進行交叉編譯，然后去編譯用SVE intrinsic方式實現的SVE測試程序，發現果然可以編過，也可以運行。編譯方法參考交叉編譯用於生成aarch64指令的GCC （9.2），這里有一份已經編譯好的：鏈接: https://pan.baidu.com/s/1s3FWLgwavaGqR427NcW-hA 提取碼: kpng

 

測試程序：

#include <stdlib.h>
#include <stdio.h>
#include <arm_sve.h>

// Scalar version.
void add_arrays(double * restrict dst, double *src, double c, const int N) {
    for (int i = 0; i < N; i++)
        dst[i] = src[i] + c;
}

// Vector version
void vla_add_arrays(double * restrict dst, double *src, double c, const int N) {
    int64_t i = 0;

    svbool_t pg = svwhilelt_b64(i, (int64_t)N);
    while (svptest_any(svptrue_b64(), pg)) {
        svfloat64_t vsrc = svld1(pg, src + i);
        svfloat64_t vdst = svadd_x(pg, vsrc, c);
        svst1(pg, dst + i, vdst);

        i += svcntd();
        pg = svwhilelt_b64(i, (int64_t)N);
    }
}

// Vector version
void vla_add_arrays_2(double *dst, double *src, double c, const int N) {
    for (int i = 0; i < N; i += svcntd()) {
        svbool_t Pg = svwhilelt_b64(i, N);
        svfloat64_t vsrc = svld1(Pg, &src[i]);
        svfloat64_t vdst = svadd_x(Pg, vsrc, c);
        svst1(Pg, &dst[i], vdst);
    }
}

int main(void) {
    double src[100];
    double c;
    double dst_serial[100], dst_vla[100], dst_vla2[100];
    for (int i = 0; i < 100; ++i) {
        src[i] = (double) i / ((double) i + 1);
    }

    c = src[rand() % 100];

    add_arrays(dst_serial, src, c, 100);
    vla_add_arrays(dst_vla, src, c, 100);
    vla_add_arrays_2(dst_vla2, src, c, 100);

    for (int i = 0; i < 100; ++i) {
        printf("%f %f %f, %f, %f\n", dst_serial[i], dst_vla[i], dst_vla2[i], src[i], c);
    }
    return 0; 
}

 

編譯：

 

CC=/home/pengdl/work/SVE/cross_compile/install/bin/aarch64-linux-gnu-gcc
CFLAGS=-g -Wall -march=armv8.2-a+sve -O1
LDFLAGS=--static

all:demo

demo:demo.o

%.o:%c

clean:
    $(RM) *.o demo

 

 

測試運行：

$ make clean;make;
rm -f *.o demo
/home/pengdl/work/SVE/cross_compile/install/bin/aarch64-linux-gnu-gcc -g -Wall -march=armv8.2-a+sve -O1   -c -o demo.o demo.c
/home/pengdl/work/SVE/cross_compile/install/bin/aarch64-linux-gnu-gcc --static  demo.o   -o demo
pengdl@pengdl-dell:~/work/SVE/cross_compile/teset
$ qemu-aarch64 ./demo
0.988095 0.988095 0.988095, 0.000000, 0.988095
1.488095 1.488095 1.488095, 0.500000, 0.988095
1.654762 1.654762 1.654762, 0.666667, 0.988095
1.738095 1.738095 1.738095, 0.750000, 0.988095
1.788095 1.788095 1.788095, 0.800000, 0.988095
1.821429 1.821429 1.821429, 0.833333, 0.988095
1.845238 1.845238 1.845238, 0.857143, 0.988095
1.863095 1.863095 1.863095, 0.875000, 0.988095
1.876984 1.876984 1.876984, 0.888889, 0.988095
1.888095 1.888095 1.888095, 0.900000, 0.988095
... ...

 

完。