Home
last modified time | relevance | path

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

/linux-6.15/lib/raid6/
H A Dloongarch_simd.c26 #define NSIZE 16 macro
52 for (d = 0; d < bytes; d += NSIZE*4) { in raid6_lsx_gen_syndrome()
235 : "+m"(p[d+NSIZE*0]), "+m"(p[d+NSIZE*1]), in raid6_lsx_xor_syndrome()
236 "+m"(p[d+NSIZE*2]), "+m"(p[d+NSIZE*3]), in raid6_lsx_xor_syndrome()
237 "+m"(q[d+NSIZE*0]), "+m"(q[d+NSIZE*1]), in raid6_lsx_xor_syndrome()
238 "+m"(q[d+NSIZE*2]), "+m"(q[d+NSIZE*3]) in raid6_lsx_xor_syndrome()
253 #undef NSIZE
257 #define NSIZE 32 macro
406 : "+m"(p[d+NSIZE*0]), "+m"(p[d+NSIZE*1]), in raid6_lasx_xor_syndrome()
407 "+m"(q[d+NSIZE*0]), "+m"(q[d+NSIZE*1]) in raid6_lasx_xor_syndrome()
[all …]
H A Dneon.uc32 #define NSIZE sizeof(unative_t)
70 for ( d = 0 ; d < bytes ; 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]);
107 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
147 w1$$ = vld1q_u8(&q[d+NSIZE*$$]);
150 vst1q_u8(&p[d+NSIZE*$$], wp$$);
[all …]
H A Dint.uc30 # define NSIZE 8
36 # define NSIZE 4
87 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
88 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
90 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
98 *(unative_t *)&p[d+NSIZE*$$] = wp$$;
99 *(unative_t *)&q[d+NSIZE*$$] = wq$$;
116 for ( d = 0 ; d < bytes ; d += NSIZE*$# ) {
120 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
135 *(unative_t *)&p[d+NSIZE*$$] ^= wp$$;
[all …]
H A 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$$;
H A 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$$;
H A Ds390vx.uc18 #define NSIZE 16
61 for (d = 0; d < bytes; d += $#*NSIZE) {
94 for (d = 0; d < bytes; d += $#*NSIZE) {