Home
last modified time | relevance | path

Searched refs:NSIZE (Results 1 – 6 of 6) sorted by relevance

/Linux-v6.6/lib/raid6/
Dloongarch_simd.c26 #define NSIZE 16 macro
52 for (d = 0; d < bytes; d += NSIZE*4) { in raid6_lsx_gen_syndrome()
54 asm volatile("vld $vr0, %0" : : "m"(dptr[z0][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
55 asm volatile("vld $vr1, %0" : : "m"(dptr[z0][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
56 asm volatile("vld $vr2, %0" : : "m"(dptr[z0][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
57 asm volatile("vld $vr3, %0" : : "m"(dptr[z0][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
64 asm volatile("vld $vr8, %0" : : "m"(dptr[z][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
65 asm volatile("vld $vr9, %0" : : "m"(dptr[z][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
66 asm volatile("vld $vr10, %0" : : "m"(dptr[z][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
67 asm volatile("vld $vr11, %0" : : "m"(dptr[z][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
[all …]
Dneon.uc32 #define NSIZE sizeof(unative_t)
70 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
71 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
73 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
82 vst1q_u8(&p[d+NSIZE*$$], wp$$);
83 vst1q_u8(&q[d+NSIZE*$$], wq$$);
101 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
102 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
103 wp$$ = veorq_u8(vld1q_u8(&p[d+$$*NSIZE]), wq$$);
107 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
[all …]
Dint.uc30 # define NSIZE 8
36 # define NSIZE 4
94 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
97 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
105 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
106 *(unative_t *)&q[d+NSIZE*$$] = wq$$;
123 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
127 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
[all …]
Dvpermxor.uc34 #define NSIZE sizeof(unative_t)
55 for (d = 0; d < bytes; d += NSIZE*$#) {
56 wp$$ = wq$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
59 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
67 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
68 *(unative_t *)&q[d+NSIZE*$$] = wq$$;
Daltivec.uc44 #define NSIZE sizeof(unative_t)
84 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
85 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
87 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
95 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
96 *(unative_t *)&q[d+NSIZE*$$] = wq$$;
Ds390vx.uc18 #define NSIZE 16
96 for (d = 0; d < bytes; d += $#*NSIZE) {
129 for (d = 0; d < bytes; d += $#*NSIZE) {