Searched refs:pbmul (Results 1 – 7 of 7) sorted by relevance
| /Linux-v4.19/lib/raid6/ |
| D | recov_avx2.c | 26 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_avx2() local
52 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_avx2()
100 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (pbmul[0])); in raid6_2data_recov_avx2()
101 asm volatile("vbroadcasti128 %0, %%ymm1" : : "m" (pbmul[16])); in raid6_2data_recov_avx2()
163 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (pbmul[0])); in raid6_2data_recov_avx2()
164 asm volatile("vbroadcasti128 %0, %%ymm1" : : "m" (pbmul[16])); in raid6_2data_recov_avx2()
|
| D | recov_avx512.c | 33 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_avx512() local
62 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_avx512()
133 : "m" (pbmul[0]), "m" (pbmul[16])); in raid6_2data_recov_avx512()
198 : "m" (pbmul[0]), "m" (pbmul[16])); in raid6_2data_recov_avx512()
|
| D | recov_ssse3.c | 26 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_ssse3() local
54 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_ssse3()
64 asm volatile("movdqa %0,%%xmm14" : : "m" (pbmul[0])); in raid6_2data_recov_ssse3()
65 asm volatile("movdqa %0,%%xmm15" : : "m" (pbmul[16])); in raid6_2data_recov_ssse3()
167 asm volatile("movdqa %0,%%xmm4" : : "m" (pbmul[0])); in raid6_2data_recov_ssse3()
168 asm volatile("movdqa %0,%%xmm1" : : "m" (pbmul[16])); in raid6_2data_recov_ssse3()
|
| D | recov_neon.c | 27 uint8_t *dq, const uint8_t *pbmul,
37 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_neon() local
64 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_neon()
69 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
|
| D | recov.c | 30 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_intx1() local
55 pbmul = raid6_gfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_intx1()
62 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ in raid6_2data_recov_intx1()
|
| D | recov_neon_inner.c | 37 uint8_t *dq, const uint8_t *pbmul, in __raid6_2data_recov_neon() argument
40 uint8x16_t pm0 = vld1q_u8(pbmul); in __raid6_2data_recov_neon()
41 uint8x16_t pm1 = vld1q_u8(pbmul + 16); in __raid6_2data_recov_neon()
|
| D | recov_s390xc.c | 27 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_s390xc() local
53 pbmul = raid6_gfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_s390xc()
61 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; in raid6_2data_recov_s390xc()
|
