使用Qemu運行Ubuntu文件系統 —— 搭建SVE學習環境（2）

開發環境

PC：ubuntu18.04

Qemu：4.1

Kernel：Linux-5.2

 

概述

　　因爲要學習ARM的SVE技術，可是目前尚未支持SVE指令的板子，因此只能用Qemu來模擬，可是發現Qemu在用戶模式下沒法設置SVE的位寬，在瀏覽ARM官網資料時發現，ARM提供了Arm Instruction Emulator（下載連接）能夠用來模擬SVE指令，而且能夠設置SVE位寬，遺憾的是該模擬器只能運行在AArch64機器上，而且提供了基於ubuntu16.04的安裝包。因此，須要先在qemu上運行一個ubuntu系統，而後再在其中安裝Arm Instruction Emulator。

 

正文

一、參考博客：使用Qemu運行Ubuntu文件系統（1）

二、參考博客：用Qemu搭建aarch64學習環境

三、參考博客：Qemu-4.1 橋接網絡設置

四、參考博客：安裝docker後，致使qemu的橋接網絡出現問題

五、下面是與上面不一樣的地方

• 使用的是qemu-aarch64-static

• 下載的ubuntu鏡像是：ubuntu-base-16.04.6-base-arm64.tar.gz

六、在運行時，使用以下命令：(下面用到的製做好的ubuntu16.04鏡像能夠到這裏下載，用戶名"pengdl"，密碼是一個空格)

sudo qemu-system-aarch64 \ -M virt \ -cpu cortex-a57 \ -smp 4 \ -m 2048M \ -kernel ./linux-5.2/arch/arm64/boot/Image \ -nographic \ -append "noinitrd root=/dev/vda rootfstype=ext4 rw" \ -nic tap \ -fsdev local,security_model=passthrough,id=fsdev0,path=/nfsroot \ -device virtio-9p-pci,id=fs1,fsdev=fsdev0,mount_tag=hostshare \ -drive if=none,file=./ubuntu_rootfs/ubuntu.ext4,id=hd0 \ -device virtio-blk-device,drive=hd0

七、系統運行起來後，能夠用使用串口或者telnet以普通用戶登陸虛擬機，而後再用mount -t nfs 或者 mount -t 9p的方式將Host上的目錄掛載到虛擬機中，來安裝ARMIE。

八、能夠參考前一篇交叉編譯支持SVE ACLE的gcc，對測試程序稍做修改，來看看修改SVE位寬的運行效果：

#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); printf("# %ld\n", i); } } // 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); printf("* %d\n", i); } } 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; }

 

運行時，能夠設置不一樣的SVE位寬：

2048：

 

 

1024：

 

 

128：

 

 

完。