Searched refs:qmul (Results 1 – 7 of 7) sorted by relevance
| /lib/raid6/ |
| D | recov_ssse3.c | 23 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_ssse3() local
51 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila] ^ in raid6_2data_recov_ssse3()
59 asm volatile("movdqa %0,%%xmm6" : : "m" (qmul[0])); in raid6_2data_recov_ssse3()
81 asm volatile("movdqa %0,%%xmm5" : : "m" (qmul[16])); in raid6_2data_recov_ssse3()
148 asm volatile("movdqa %0,%%xmm4" : : "m" (qmul[0])); in raid6_2data_recov_ssse3()
149 asm volatile("movdqa %0,%%xmm5" : : "m" (qmul[16])); in raid6_2data_recov_ssse3()
197 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_ssse3() local
218 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_ssse3()
229 asm volatile("movdqa %0, %%xmm0" : : "m" (qmul[0])); in raid6_datap_recov_ssse3()
234 asm volatile("movdqa %0, %%xmm1" : : "m" (qmul[16])); in raid6_datap_recov_ssse3()
[all …]
|
| D | recov_avx2.c | 23 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_avx2() local
49 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila] ^ in raid6_2data_recov_avx2()
75 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (qmul[0])); in raid6_2data_recov_avx2()
76 asm volatile("vbroadcasti128 %0, %%ymm5" : : "m" (qmul[16])); in raid6_2data_recov_avx2()
143 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (qmul[0])); in raid6_2data_recov_avx2()
144 asm volatile("vbroadcasti128 %0, %%ymm5" : : "m" (qmul[16])); in raid6_2data_recov_avx2()
192 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_avx2() local
211 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_avx2()
228 asm volatile("vbroadcasti128 %0, %%ymm0" : : "m" (qmul[0])); in raid6_datap_recov_avx2()
230 asm volatile("vbroadcasti128 %0, %%ymm1" : : "m" (qmul[16])); in raid6_datap_recov_avx2()
[all …]
|
| D | recov_avx512.c | 29 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_avx512() local
58 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila] ^ in raid6_2data_recov_avx512()
91 : "m" (qmul[0]), "m" (qmul[16])); in raid6_2data_recov_avx512()
173 : "m" (qmul[0]), "m" (qmul[16])); in raid6_2data_recov_avx512()
231 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_avx512() local
253 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_avx512()
278 : "m" (qmul[0]), "m" (qmul[16])); in raid6_datap_recov_avx512()
334 : "m" (qmul[0]), "m" (qmul[16])); in raid6_datap_recov_avx512()
|
| D | recov_neon.c | 24 const uint8_t *qmul);
27 const uint8_t *qmul);
34 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_neon() local
61 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila] ^ in raid6_2data_recov_neon()
65 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
73 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_neon() local
93 qmul = raid6_vgfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_neon()
96 __raid6_datap_recov_neon(bytes, p, q, dq, qmul); in raid6_datap_recov_neon()
|
| D | recov_neon_inner.c | 29 const uint8_t *qmul) in __raid6_2data_recov_neon() argument
33 uint8x16_t qm0 = vld1q_u8(qmul); in __raid6_2data_recov_neon()
34 uint8x16_t qm1 = vld1q_u8(qmul + 16); in __raid6_2data_recov_neon()
78 const uint8_t *qmul) in __raid6_datap_recov_neon() argument
80 uint8x16_t qm0 = vld1q_u8(qmul); in __raid6_datap_recov_neon()
81 uint8x16_t qm1 = vld1q_u8(qmul + 16); in __raid6_datap_recov_neon()
|
| D | recov.c | 26 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_intx1() local
51 qmul = raid6_gfmul[raid6_gfinv[raid6_gfexp[faila]^raid6_gfexp[failb]]]; in raid6_2data_recov_intx1()
56 qx = qmul[*q ^ *dq]; in raid6_2data_recov_intx1()
68 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_intx1() local
86 qmul = raid6_gfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_intx1()
90 *p++ ^= *dq = qmul[*q ^ *dq]; in raid6_datap_recov_intx1()
|
| D | recov_s390xc.c | 28 const u8 *qmul; /* Q multiplier table (for both) */ in raid6_2data_recov_s390xc() local
54 qmul = raid6_gfmul[raid6_gfinv[raid6_gfexp[faila]^raid6_gfexp[failb]]]; in raid6_2data_recov_s390xc()
61 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; in raid6_2data_recov_s390xc()
76 const u8 *qmul; /* Q multiplier table */ in raid6_datap_recov_s390xc() local
95 qmul = raid6_gfmul[raid6_gfinv[raid6_gfexp[faila]]]; in raid6_datap_recov_s390xc()
101 dq[i] = qmul[dq[i]]; in raid6_datap_recov_s390xc()
|