令初始数据为:

float d0[4] = {0.f, 1.f, 2.f, 3.f};
float d1[4] = {4.f, 5.f, 6.f, 7.f};
float d2[4] = {8.f, 9.f, 10.f, 11.f};
float d3[4] = {12.f, 13.f, 14.f, 15.f};

一、基本的加载存储操作

1. vld1q_f32

float32x4_t q0 = vld1q_f32(d0); // 加载 d0 地址起始的 4 个 float 数据到 q0

NEON 常用函数及其执行结果_寄存器

2.vst1q_f32

vst1q_f32(d1, q0);// 将 q0 中 4 个 float32,赋值给以 d1 为起始地址的 4 个 float32

 NEON 常用函数及其执行结果_d3_02NEON 常用函数及其执行结果_寄存器_03

 3.vld2q_f32 

float d4[8]= {1.f, 2.f, 3.f, 4.f, 5.f, 6.f, 7.f, 8.f};
float32x4x2_t ret = vld2q_f32 (d4);

 NEON 常用函数及其执行结果_d3_04

注意,此时在寄存器是交错读取的!

 4.vst2q_f32

vst2q_f32 (d4, ret);

 NEON 常用函数及其执行结果_数据_05

注意,由于寄存器是交错存储的,所以内存保持不变!

5.vld3q_f32

float d5[12] = {1.f, 2.f, 3.f, 4.f,
5.f, 6.f, 7.f, 8.f,
9.f, 10.f, 11.f, 12.f};
float32x4x3_t f = vld3q_f32 (d5);

 NEON 常用函数及其执行结果_寄存器_06

6.vst3q_f32

vst3q_f32 (d5, f);

NEON 常用函数及其执行结果_寄存器_07

7.vld4q_f32, vst4q_f32

略 

二、特殊操作 

 1.vdupq_n_f32

float32x4_t res = vdupq_n_f32(0.f); // 存储的四个 float32 都初始化为 0

NEON 常用函数及其执行结果_数据_08

2.vzipq_f32 

float32x4x2_t q4 = vzipq_f32 (q0, q1);

NEON 常用函数及其执行结果_寄存器_09

 3.vuzpq_f32

float32x4x2_t ret = vuzpq_f32 (q0, q1);

 NEON 常用函数及其执行结果_数据_10

 可见,打包 (zip)、拆包(unzip)并不是想当然的可逆的运算

4.vcombine_f32 

float32x2_t a = vget_low_f32(q0);
float32x2_t b = vget_high_f32(q0);
float32x4_t ret = vcombine_f32 (a, b);

NEON 常用函数及其执行结果_数据_11

5. vget_low_f32

float32x2_t low = vget_low_f32(q0); // 取低2位

 NEON 常用函数及其执行结果_d3_12

6. vget_high_f32

float32x2_t high = vget_high_f32(q0); // 取高2位

 NEON 常用函数及其执行结果_d3_13

7. vtrnq_f32

float32x4x2_t ret = vtrnq_f32 (q0, q1)

NEON 常用函数及其执行结果_数据_14 NEON 常用函数及其执行结果_d3_15


8. vextq_f32

// 拼接两个寄存器并返回从第 n 位开始的大小为4的寄存器 0<=n<=3 
res = vextq_f32(q0, q1, 2); //取 q1 低2位,拼接到 q0 的高位,保留 q0 的高2位(移到低位)
// q0, q1 实际数据没有变化

NEON 常用函数及其执行结果_数据_16NEON 常用函数及其执行结果_数据_17

  •  vext_u8 的例子:
uint8x8_t ret = vext_u8 (p, q, 2); // 取 q 的低两位作为 p 的高位,p 向左移动两位腾出空间

NEON 常用函数及其执行结果_数据_18

9.vget_lane_f32

float lane0 = vget_lane_f32(ss0, 0);// get 0th parameter in vector

 NEON 常用函数及其执行结果_数据_19NEON 常用函数及其执行结果_寄存器_20


10. vsetq_lane_f32

float32x4_t res = vsetq_lane_f32(d1[0], q1, 1);//用 d1[0] 的数据替换掉 q1[1](q1 实际数据没有变化)

NEON 常用函数及其执行结果_d3_21NEON 常用函数及其执行结果_数据_22

11.vtbl1_s8

int8x8_t r = vtbl1_s8 (p, q);

NEON 常用函数及其执行结果_d3_23

12.vrev16_s8

int8x8_t s = vrev16_s8 (q);

 NEON 常用函数及其执行结果_d3_24NEON 常用函数及其执行结果_寄存器_25

 三、基本数据类型的转换

1.vcvtq_u32_f32

uint32x4_t ui0 = vcvtq_u32_f32 (q0);

NEON 常用函数及其执行结果_数据_26

2.vcvtq_s32_f32 

int32x4_t i0 = vcvtq_s32_f32 (q1);

NEON 常用函数及其执行结果_寄存器_27

3. vcvtq_f32_s32

float32x4_t f0 = vcvtq_f32_s32 (i0);

 NEON 常用函数及其执行结果_寄存器_28

4.vcvtq_f32_u32

float32x4_t uf0 = vcvtq_f32_u32 (ui0)

NEON 常用函数及其执行结果_数据_29

四、基本比较运算

1.vceq_f32  

uint32x2_t c = vceq_f32 (a, b); // 等于

NEON 常用函数及其执行结果_数据_30

2.vceqq_f32

uint32x4_t q = vceqq_f32 (q1, q2); // 等于

 NEON 常用函数及其执行结果_d3_31NEON 常用函数及其执行结果_数据_32

3. vmaxq_f32


float32x4_t ret = vmaxq_f32 (q2, q1);

NEON 常用函数及其执行结果_寄存器_33NEON 常用函数及其执行结果_寄存器_34

4. vminq_f32


float32x4_t ret0 = vminq_f32 (q2, q1);

NEON 常用函数及其执行结果_d3_35 NEON 常用函数及其执行结果_数据_36

5.vpmax_s8

int8x8_t r = vpmax_s8 (p, q);

NEON 常用函数及其执行结果_d3_37 NEON 常用函数及其执行结果_d3_38

6.vpmin_s8

int8x8_t s = vpmin_s8 (p, q);

 NEON 常用函数及其执行结果_数据_39NEON 常用函数及其执行结果_寄存器_40

五、基本的位运算

 1.vclsq_s32

int32x4_t q1 = vclsq_s32 (q0); // 统计和符号位相同的 bit 数(不包括符号位)

NEON 常用函数及其执行结果_d3_41NEON 常用函数及其执行结果_d3_42

 2.vclzq_s32

int32x4_t q2 = vclzq_s32 (q0); // 统计前缀 0 的个数

NEON 常用函数及其执行结果_寄存器_43 NEON 常用函数及其执行结果_寄存器_44

3.vcnt_s8

int8_t d0[8] = {0, 1, 2, 3, 4, 5, 6, 7};
int8x8_t q = vld1_s8(d0);
int8x8_t p = vcnt_s8 (q); // 二进制形式的 1 的个数

 NEON 常用函数及其执行结果_寄存器_45

4.vmvn_s8 

int8x8_t q = vmvn_s8 (p); // 按位取反

 NEON 常用函数及其执行结果_数据_46 

5.vqneg_s8 

int8x8_t r = vqneg_s8 (p);

NEON 常用函数及其执行结果_数据_47 NEON 常用函数及其执行结果_数据_48

6. vqshl_s8

int8_t d0[8] = {0, 1, 2, 3, 4, 5, 6, 7};
int8_t d1[8] = {1, 1, 2, 2, 3, 3, 4, 4};
int8x8_t p = vld1_s8(d0);
int8x8_t q = vld1_s8(d1);
int8x8_t pq = vqshl_s8 (p, q); // 左移对应的位数

NEON 常用函数及其执行结果_寄存器_49

如果移位是负数 ,则变成截断的右移

int8_t d0[8] = {0, 1, 2, 3, 4, 5, 6, 7};
int8_t d1[8] = {-1, -1, -2, -2, -3, -3, -4, -4};
int8x8_t p = vld1_s8(d0);
int8x8_t q = vld1_s8(d1);
int8x8_t pq = vqshl_s8 (p, q);

 NEON 常用函数及其执行结果_数据_50


六、基本的逻辑运算

 略

 七、基本的算术运算

1.vadd_f32

float32x2_t ss0 = vadd_f32(vget_low_f32(q2), vget_high_f32(q2));//对应元素相加

 NEON 常用函数及其执行结果_寄存器_20

2.vaddq_f32

float32x4_t q4 = vaddq_f32 (q1, q2);

 NEON 常用函数及其执行结果_寄存器_52NEON 常用函数及其执行结果_寄存器_53

3.vpadd_f32

float32x2_t ss1 = vpadd_f32(vget_low_f32(q2), vget_high_f32(q2));//相邻元素相加

NEON 常用函数及其执行结果_寄存器_54

3.vmulq_f32

float32x4_t res0 = vmulq_f32(q0, q1); //点乘

 NEON 常用函数及其执行结果_寄存器_55NEON 常用函数及其执行结果_d3_56

4. vmlaq_f32

float32x4_t res1 = vmlaq_f32(q0, q1, q2);// q0 + q1*q2

NEON 常用函数及其执行结果_d3_57 NEON 常用函数及其执行结果_寄存器_58


5.vmlaq_lane_f32

//  ri = ai + bi * c[d];
float32x4_t res = vmlaq_lane_f32(q0, q1, vget_low_f32(q2), 0);//取 q2 的第0个数,分别与 q1 中的 4 个数相乘,得到 4 个结果与 q0 累加

NEON 常用函数及其执行结果_寄存器_59NEON 常用函数及其执行结果_数据_60


6.vmaxq_f3

float32x4_t max = vmaxq_f32(q1, q2);//对应元素比较,取最大

 NEON 常用函数及其执行结果_d3_61NEON 常用函数及其执行结果_数据_60

 7.vrecpeq_f32

float32x4_t q5 = vrecpeq_f32 (q1); // 倒数

NEON 常用函数及其执行结果_数据_63

 8.vrsqrteq_f32

float32x4_t q6 = vrsqrteq_f32 (q1); // 倒数平方根

NEON 常用函数及其执行结果_d3_64

待续