Searched refs:pbmul (Results 1 – 7 of 7) sorted by relevance
| /kernel/linux/linux-5.10/lib/raid6/ |
| D | recov_avx2.c | 20 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_avx2() local
46 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_avx2()
94 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (pbmul[0])); in raid6_2data_recov_avx2()
95 asm volatile("vbroadcasti128 %0, %%ymm1" : : "m" (pbmul[16])); in raid6_2data_recov_avx2()
157 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (pbmul[0])); in raid6_2data_recov_avx2()
158 asm volatile("vbroadcasti128 %0, %%ymm1" : : "m" (pbmul[16])); in raid6_2data_recov_avx2()
|
| D | recov_ssse3.c | 20 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_ssse3() local
48 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_ssse3()
58 asm volatile("movdqa %0,%%xmm14" : : "m" (pbmul[0])); in raid6_2data_recov_ssse3()
59 asm volatile("movdqa %0,%%xmm15" : : "m" (pbmul[16])); in raid6_2data_recov_ssse3()
161 asm volatile("movdqa %0,%%xmm4" : : "m" (pbmul[0])); in raid6_2data_recov_ssse3()
162 asm volatile("movdqa %0,%%xmm1" : : "m" (pbmul[16])); in raid6_2data_recov_ssse3()
|
| D | recov_avx512.c | 28 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_avx512() local
57 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_avx512()
128 : "m" (pbmul[0]), "m" (pbmul[16])); in raid6_2data_recov_avx512()
193 : "m" (pbmul[0]), "m" (pbmul[16])); in raid6_2data_recov_avx512()
|
| D | recov_neon.c | 23 uint8_t *dq, const uint8_t *pbmul,
33 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_neon() local
60 pbmul = raid6_vgfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_neon()
65 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
|
| D | recov.c | 25 const u8 *pbmul; /* P multiplier table for B data */ in raid6_2data_recov_intx1() local
50 pbmul = raid6_gfmul[raid6_gfexi[failb-faila]]; in raid6_2data_recov_intx1()
57 *dq++ = db = pbmul[px] ^ qx; /* Reconstructed B */ in raid6_2data_recov_intx1()
|
| 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()
|
| D | recov_neon_inner.c | 28 uint8_t *dq, const uint8_t *pbmul, in __raid6_2data_recov_neon() argument
31 uint8x16_t pm0 = vld1q_u8(pbmul); in __raid6_2data_recov_neon()
32 uint8x16_t pm1 = vld1q_u8(pbmul + 16); in __raid6_2data_recov_neon()
|