718c41634f
1.项目后端整体迁移至PaddleOCR-NCNN算法，已通过基本的兼容性测试 2.工程改为使用CMake组织，后续为了更好地兼容第三方库，不再提供QMake工程 3.重整权利声明文件，重整代码工程，确保最小化侵权风险 Log: 切换后端至PaddleOCR-NCNN，切换工程为CMake Change-Id: I4d5d2c5d37505a4a24b389b1a4c5d12f17bfa38c
131 lines
2.7 KiB
Markdown
131 lines
2.7 KiB
Markdown
```c
|
||
// d寄存器全部使用 %P
|
||
// d reg matches %P
|
||
// a += b * c
|
||
float32x2_t _a = vld1_f32(a);
|
||
float32x2_t _b = vld1_f32(b);
|
||
float32x2_t _c = vld1_f32(c);
|
||
asm volatile(
|
||
"vmla.f32 %P0, %P2, %P3"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// q寄存器全部使用 %q
|
||
// q reg matches %q
|
||
// a += b * c
|
||
float32x4_t _a = vld1q_f32(a);
|
||
float32x4_t _b = vld1q_f32(b);
|
||
float32x4_t _c = vld1q_f32(c);
|
||
asm volatile(
|
||
"vmla.f32 %q0, %q2, %q3"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// d寄存器单路使用 %P[0] %P[1]
|
||
// 32bit d reg matches %P[0]
|
||
// a += b * c[0]
|
||
// a += b * c[1]
|
||
float32x2_t _a = vld1_f32(a);
|
||
float32x2_t _b = vld1_f32(b);
|
||
float32x2_t _c = vld1_f32(c);
|
||
asm volatile(
|
||
"vmla.f32 %P0, %P2, %P3[0]"
|
||
"vmla.f32 %P0, %P2, %P3[1]"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// q寄存器单路使用 %e[0] %e[1] %f[0] %f[1]
|
||
// 32-bit q reg matches %e[0]
|
||
// a += b * c[0]
|
||
// a += b * c[1]
|
||
// a += b * c[2]
|
||
// a += b * c[3]
|
||
float32x4_t _a = vld1q_f32(a);
|
||
float32x4_t _b = vld1q_f32(b);
|
||
float32x4_t _c = vld1q_f32(c);
|
||
asm volatile(
|
||
"vmla.f32 %q0, %q2, %e3[0]"
|
||
"vmla.f32 %q0, %q2, %e3[1]"
|
||
"vmla.f32 %q0, %q2, %f3[0]"
|
||
"vmla.f32 %q0, %q2, %f3[1]"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// q寄存器拆分d寄存器使用 %e %f
|
||
// use %e %f to split q reg into two d regs
|
||
// a += b * c[0]c[1]
|
||
// a += b * c[2]c[3]
|
||
float32x2_t _a = vldq_f32(a);
|
||
float32x2_t _b = vldq_f32(b);
|
||
float32x4_t _c = vld1q_f32(c);
|
||
asm volatile(
|
||
"vmla.f32 %P0, %P2, %e3"
|
||
"vmla.f32 %P0, %P2, %f3"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// d寄存器声明绑定
|
||
// specify concrete d reg which want to save
|
||
// vmla.f32 d0, d2, d4
|
||
register float32x2_t _a asm("d0") = vld1_f32(a);
|
||
register float32x2_t _b asm("d2") = vld1_f32(b);
|
||
register float32x2_t _c asm("d4") = vld1_f32(c);
|
||
|
||
asm volatile(
|
||
"vmla.f32 %P0, %P2, %P3"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
```c
|
||
// q寄存器声明绑定
|
||
// bind q reg with data
|
||
// vmla.f32 q0, q1, q2
|
||
register float32x4_t _a asm("q0") = vld1q_f32(a);
|
||
register float32x4_t _b asm("q1") = vld1q_f32(b);
|
||
register float32x4_t _c asm("q2") = vld1q_f32(c);
|
||
|
||
asm volatile(
|
||
"vmla.f32 %q0, %q2, %q3"
|
||
: "=w"(_a) // %0
|
||
: "0"(_a),
|
||
"w"(_b), // %2
|
||
"w"(_c) // %3
|
||
:
|
||
);
|
||
```
|
||
|
||
如果不是因为编译器的bug，寄存器绑定是用不着的，然而。。。
|
||
|
||
https://gcc.gnu.org/bugzilla/show_bug.cgi?id=41538
|
||
|
||
qwq
|