| /lib/ |
| A D | asn1_decoder.c | 67 if (datalen == dp) in asn1_find_indefinite_length()
73 tag = data[dp++]; in asn1_find_indefinite_length()
80 *_dp = dp; in asn1_find_indefinite_length()
95 len = data[dp++]; in asn1_find_indefinite_length()
120 dp += len; in asn1_find_indefinite_length()
138 *_dp = dp; in asn1_find_indefinite_length()
252 dp--; in asn1_ber_decoder()
307 tdp = dp; in asn1_ber_decoder()
352 dp += len; in asn1_ber_decoder()
408 dp--; in asn1_ber_decoder()
[all …]
|
| A D | dynamic_debug.c | 230 if (p != dp->format) in ddebug_change()
247 if (newflags == dp->flags) in ddebug_change()
258 trim_prefix(dp->filename), dp->lineno, in ddebug_change()
262 dp->flags = newflags; in ddebug_change()
1079 struct _ddebug *dp; in ddebug_proc_start() local
1088 dp = ddebug_iter_first(iter); in ddebug_proc_start()
1091 return dp; in ddebug_proc_start()
1102 struct _ddebug *dp; in ddebug_proc_next() local
1109 return dp; in ddebug_proc_next()
1135 struct _ddebug *dp = p; in ddebug_proc_show() local
[all …]
|
| /lib/raid6/ |
| A D | recov_loongarch_simd.c | 32 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lsx() local
44 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_lsx()
46 ptrs[disks - 2] = dp; in raid6_2data_recov_lsx()
54 ptrs[faila] = dp; in raid6_2data_recov_lsx()
95 asm volatile("vld $vr8, %0" : : "m" (dp[0])); in raid6_2data_recov_lsx()
179 dp += 64; in raid6_2data_recov_lsx()
306 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lasx() local
318 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_lasx()
320 ptrs[disks - 2] = dp; in raid6_2data_recov_lasx()
328 ptrs[faila] = dp; in raid6_2data_recov_lasx()
[all …]
|
| A D | recov_avx2.c | 19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx2() local
30 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_avx2()
32 ptrs[disks-2] = dp; in raid6_2data_recov_avx2()
40 ptrs[faila] = dp; in raid6_2data_recov_avx2()
63 asm volatile("vpxor %0, %%ymm0, %%ymm0" : : "m" (dp[0])); in raid6_2data_recov_avx2()
125 asm volatile("vmovdqa %%ymm0, %0" : "=m" (dp[0])); in raid6_2data_recov_avx2()
126 asm volatile("vmovdqa %%ymm8, %0" : "=m" (dp[32])); in raid6_2data_recov_avx2()
131 dp += 64; in raid6_2data_recov_avx2()
137 asm volatile("vpxor %0, %%ymm0, %%ymm0" : : "m" (*dp)); in raid6_2data_recov_avx2()
173 asm volatile("vmovdqa %%ymm0, %0" : "=m" (dp[0])); in raid6_2data_recov_avx2()
[all …]
|
| A D | recov_avx512.c | 25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx512() local
39 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_avx512()
41 ptrs[disks-2] = dp; in raid6_2data_recov_avx512()
49 ptrs[faila] = dp; in raid6_2data_recov_avx512()
77 "m" (dp[0]), "m" (dp[64])); in raid6_2data_recov_avx512()
151 : "m" (dp[0]), "m" (dp[64])); in raid6_2data_recov_avx512()
156 dp += 128; in raid6_2data_recov_avx512()
164 : "m" (*q), "m" (*p), "m"(*dq), "m" (*dp)); in raid6_2data_recov_avx512()
212 : "m" (dp[0])); in raid6_2data_recov_avx512()
217 dp += 64; in raid6_2data_recov_avx512()
|
| A D | recov_ssse3.c | 19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_ssse3() local
32 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_ssse3()
34 ptrs[disks-2] = dp; in raid6_2data_recov_ssse3()
42 ptrs[faila] = dp; in raid6_2data_recov_ssse3()
73 asm volatile("pxor %0,%%xmm0" : : "m" (dp[0])); in raid6_2data_recov_ssse3()
74 asm volatile("pxor %0,%%xmm8" : : "m" (dp[16])); in raid6_2data_recov_ssse3()
129 asm volatile("movdqa %%xmm0,%0" : "=m" (dp[0])); in raid6_2data_recov_ssse3()
135 dp += 32; in raid6_2data_recov_ssse3()
141 asm volatile("pxor %0,%%xmm0" : : "m" (*dp)); in raid6_2data_recov_ssse3()
177 asm volatile("movdqa %%xmm0,%0" : "=m" (*dp)); in raid6_2data_recov_ssse3()
[all …]
|
| A D | recov_rvv.c | 17 static void __raid6_2data_recov_rvv(int bytes, u8 *p, u8 *q, u8 *dp, in __raid6_2data_recov_rvv() argument
79 [dp]"r"(dp), in __raid6_2data_recov_rvv()
91 dp += 16; in __raid6_2data_recov_rvv()
155 u8 *p, *q, *dp, *dq; in raid6_2data_recov_rvv() local
167 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_rvv()
169 ptrs[disks - 2] = dp; in raid6_2data_recov_rvv()
177 ptrs[faila] = dp; in raid6_2data_recov_rvv()
188 __raid6_2data_recov_rvv(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_rvv()
|
| A D | recov_s390xc.c | 25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_s390xc() local
36 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_s390xc()
38 ptrs[disks-2] = dp; in raid6_2data_recov_s390xc()
46 ptrs[faila] = dp; in raid6_2data_recov_s390xc()
57 xor_block(dp, p); in raid6_2data_recov_s390xc()
60 dq[i] = pbmul[dp[i]] ^ qmul[dq[i]]; in raid6_2data_recov_s390xc()
61 xor_block(dp, dq); in raid6_2data_recov_s390xc()
64 dp += 256; in raid6_2data_recov_s390xc()
|
| A D | recov.c | 22 u8 *p, *q, *dp, *dq; in raid6_2data_recov_intx1() local
33 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_intx1()
35 ptrs[disks-2] = dp; in raid6_2data_recov_intx1()
43 ptrs[faila] = dp; in raid6_2data_recov_intx1()
54 px = *p ^ *dp; in raid6_2data_recov_intx1()
57 *dp++ = db ^ px; /* Reconstructed A */ in raid6_2data_recov_intx1()
|
| A D | recov_neon.c | 26 u8 *p, *q, *dp, *dq; in raid6_2data_recov_neon() local
38 dp = (u8 *)ptrs[faila]; in raid6_2data_recov_neon()
40 ptrs[disks - 2] = dp; in raid6_2data_recov_neon()
48 ptrs[faila] = dp; in raid6_2data_recov_neon()
59 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
|
| A D | recov_neon_inner.c | 28 void __raid6_2data_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dp, in __raid6_2data_recov_neon() argument
53 px = veorq_u8(vld1q_u8(p), vld1q_u8(dp)); in __raid6_2data_recov_neon()
68 vst1q_u8(dp, veorq_u8(db, px)); in __raid6_2data_recov_neon()
73 dp += 16; in __raid6_2data_recov_neon()
|
| A D | neon.h | 15 void __raid6_2data_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dp,
|
| /lib/crypto/mpi/ |
| A D | mpi-div.c | 63 mpi_ptr_t np, dp; in mpi_tdiv_qr() local
110 dp = den->d; in mpi_tdiv_qr()
118 rlimb = mpihelp_divmod_1(qp, np, nsize, dp[0]); in mpi_tdiv_qr()
123 rlimb = mpihelp_mod_1(np, nsize, dp[0]); in mpi_tdiv_qr()
146 normalization_steps = count_leading_zeros(dp[dsize - 1]); in mpi_tdiv_qr()
163 mpihelp_lshift(tp, dp, dsize, normalization_steps); in mpi_tdiv_qr()
164 dp = tp; in mpi_tdiv_qr()
180 if (dp == rp || (quot && (dp == qp))) { in mpi_tdiv_qr()
186 MPN_COPY(tp, dp, dsize); in mpi_tdiv_qr()
187 dp = tp; in mpi_tdiv_qr()
[all …]
|
| A D | mpih-div.c | 190 mpi_ptr_t np, mpi_size_t nsize, mpi_ptr_t dp, mpi_size_t dsize) in mpihelp_divrem() argument
210 d = dp[0]; in mpihelp_divrem()
237 d1 = dp[1]; in mpihelp_divrem()
238 d0 = dp[0]; in mpihelp_divrem()
301 dX = dp[dsize - 1]; in mpihelp_divrem()
302 d1 = dp[dsize - 2]; in mpihelp_divrem()
307 || mpihelp_cmp(np, dp, dsize - 1) >= 0) { in mpihelp_divrem()
308 mpihelp_sub_n(np, np, dp, dsize); in mpihelp_divrem()
353 cy_limb = mpihelp_submul_1(np, dp, dsize, q); in mpihelp_divrem()
356 mpihelp_add_n(np, np, dp, dsize); in mpihelp_divrem()
|
| A D | mpi-internal.h | 192 mpi_ptr_t dp, mpi_size_t dsize);
|
| /lib/math/ |
| A D | rational.c | 58 unsigned long dp, a; in rational_best_approximation() local
65 dp = d; in rational_best_approximation()
68 n = dp; in rational_best_approximation()
94 if (!d1 || 2u * t > a || (2u * t == a && d0 * dp > d1 * d)) { in rational_best_approximation()
|