Home
last modified time | relevance | path

Searched refs:pbmul (Results 1 – 7 of 7) sorted by relevance

/linux-6.1.9/lib/raid6/
Drecov_avx2.c20 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()
Drecov_avx512.c28 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()
Drecov_ssse3.c20 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()
Drecov_neon.c23 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()
Drecov_s390xc.c27 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()
Drecov.c25 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()
Drecov_neon_inner.c28 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()