Home
last modified time | relevance | path

Searched refs:q (Results 1 – 25 of 45) sorted by relevance

12

/lib/crypto/
A Dgf128mul.c58 q(0x00), q(0x01), q(0x02), q(0x03), q(0x04), q(0x05), q(0x06), q(0x07),\
59 q(0x08), q(0x09), q(0x0a), q(0x0b), q(0x0c), q(0x0d), q(0x0e), q(0x0f),\
60 q(0x10), q(0x11), q(0x12), q(0x13), q(0x14), q(0x15), q(0x16), q(0x17),\
61 q(0x18), q(0x19), q(0x1a), q(0x1b), q(0x1c), q(0x1d), q(0x1e), q(0x1f),\
62 q(0x20), q(0x21), q(0x22), q(0x23), q(0x24), q(0x25), q(0x26), q(0x27),\
63 q(0x28), q(0x29), q(0x2a), q(0x2b), q(0x2c), q(0x2d), q(0x2e), q(0x2f),\
64 q(0x30), q(0x31), q(0x32), q(0x33), q(0x34), q(0x35), q(0x36), q(0x37),\
65 q(0x38), q(0x39), q(0x3a), q(0x3b), q(0x3c), q(0x3d), q(0x3e), q(0x3f),\
66 q(0x40), q(0x41), q(0x42), q(0x43), q(0x44), q(0x45), q(0x46), q(0x47),\
67 q(0x48), q(0x49), q(0x4a), q(0x4b), q(0x4c), q(0x4d), q(0x4e), q(0x4f),\
[all …]
/lib/
A Dlwq.c23 if (lwq_empty(q)) in __lwq_dequeue()
25 spin_lock(&q->lock); in __lwq_dequeue()
26 this = q->ready; in __lwq_dequeue()
32 q->ready = NULL; in __lwq_dequeue()
53 if (lwq_empty(q)) in lwq_dequeue_all()
57 r = q->ready; in lwq_dequeue_all()
58 q->ready = NULL; in lwq_dequeue_all()
89 wait_var_event(q, (t = lwq_dequeue(q, struct tnode, n)) != NULL); in lwq_exercise()
92 wake_up_var(q); in lwq_exercise()
102 struct lwq q; in lwq_test() local
[all …]
A Dts_kmp.c45 unsigned int i, q = 0, text_len, consumed = state->offset; in kmp_find() local
56 while (q > 0 && kmp->pattern[q] in kmp_find()
58 q = kmp->prefix_tbl[q - 1]; in kmp_find()
59 if (kmp->pattern[q] in kmp_find()
61 q++; in kmp_find()
62 if (unlikely(q == kmp->pattern_len)) { in kmp_find()
77 unsigned int k, q; in compute_prefix_tbl() local
80 for (k = 0, q = 1; q < len; q++) { in compute_prefix_tbl()
82 != (icase ? toupper(pattern[q]) : pattern[q])) in compute_prefix_tbl()
85 == (icase ? toupper(pattern[q]) : pattern[q])) in compute_prefix_tbl()
[all …]
A Dstring_helpers.c192 switch (*q) { in unescape_space()
221 if (isodigit(*q) == 0) in unescape_octal()
224 num = (*q++) & 7; in unescape_octal()
225 while (num < 32 && isodigit(*q) && (q - *src < 3)) { in unescape_octal()
227 num += (*q++) & 7; in unescape_octal()
231 *src = q; in unescape_octal()
241 if (*q++ != 'x') in unescape_hex()
248 digit = hex_to_bin(*q); in unescape_hex()
250 q++; in unescape_hex()
255 *src = q; in unescape_hex()
[all …]
/lib/raid6/
A Davx2.c37 u8 *p, *q; in raid6_avx21_gen_syndrome() local
42 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
86 u8 *p, *q; in raid6_avx21_xor_syndrome() local
91 q = dptr[disks-1]; /* RS syndrome */ in raid6_avx21_xor_syndrome()
144 u8 *p, *q; in raid6_avx22_gen_syndrome() local
149 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx22_gen_syndrome()
196 u8 *p, *q; in raid6_avx22_xor_syndrome() local
201 q = dptr[disks-1]; /* RS syndrome */ in raid6_avx22_xor_syndrome()
276 u8 *p, *q; in raid6_avx24_gen_syndrome() local
281 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx24_gen_syndrome()
[all …]
A Dsse2.c39 u8 *p, *q; in raid6_sse21_gen_syndrome() local
44 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse21_gen_syndrome()
91 u8 *p, *q; in raid6_sse21_xor_syndrome() local
96 q = dptr[disks-1]; /* RS syndrome */ in raid6_sse21_xor_syndrome()
149 u8 *p, *q; in raid6_sse22_gen_syndrome() local
154 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse22_gen_syndrome()
202 u8 *p, *q; in raid6_sse22_xor_syndrome() local
207 q = dptr[disks-1]; /* RS syndrome */ in raid6_sse22_xor_syndrome()
281 u8 *p, *q; in raid6_sse24_gen_syndrome() local
286 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse24_gen_syndrome()
[all …]
A Drecov_loongarch_simd.c32 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lsx() local
57 ptrs[disks - 1] = q; in raid6_2data_recov_lsx()
178 q += 64; in raid6_2data_recov_lsx()
189 u8 *p, *q, *dq; in raid6_datap_recov_lsx() local
207 ptrs[disks - 1] = q; in raid6_datap_recov_lsx()
281 q += 64; in raid6_datap_recov_lsx()
306 u8 *p, *q, *dp, *dq; in raid6_2data_recov_lasx() local
331 ptrs[disks - 1] = q; in raid6_2data_recov_lasx()
417 q += 64; in raid6_2data_recov_lasx()
428 u8 *p, *q, *dq; in raid6_datap_recov_lasx() local
[all …]
A Davx512.c45 u8 *p, *q; in raid6_avx5121_gen_syndrome() local
103 u8 *p, *q; in raid6_avx5121_xor_syndrome() local
172 u8 *p, *q; in raid6_avx5122_gen_syndrome() local
235 u8 *p, *q; in raid6_avx5122_xor_syndrome() local
307 : "m" (q[d]), "m" (q[d+64]), "m" (p[d]), in raid6_avx5122_xor_syndrome()
331 u8 *p, *q; in raid6_avx5124_gen_syndrome() local
413 "m" (p[d+192]), "m" (q[d]), "m" (q[d+64]), in raid6_avx5124_gen_syndrome()
414 "m" (q[d+128]), "m" (q[d+192])); in raid6_avx5124_gen_syndrome()
425 u8 *p, *q; in raid6_avx5124_xor_syndrome() local
503 : "m" (q[d]), "m" (q[d+128])); in raid6_avx5124_xor_syndrome()
[all …]
A Drvv.c29 u8 *p, *q; in raid6_rvv1_gen_syndrome_real() local
35 q = dptr[z0 + 2]; /* RS syndrome */ in raid6_rvv1_gen_syndrome_real()
93 [wq0]"r"(&q[d + NSIZE * 0]) in raid6_rvv1_gen_syndrome_real()
102 u8 *p, *q; in raid6_rvv1_xor_syndrome_real() local
192 [wq0]"r"(&q[d + NSIZE * 0]) in raid6_rvv1_xor_syndrome_real()
200 u8 *p, *q; in raid6_rvv2_gen_syndrome_real() local
292 u8 *p, *q; in raid6_rvv2_xor_syndrome_real() local
420 u8 *p, *q; in raid6_rvv4_gen_syndrome_real() local
546 u8 *p, *q; in raid6_rvv4_xor_syndrome_real() local
730 u8 *p, *q; in raid6_rvv8_gen_syndrome_real() local
[all …]
A Drecov_avx2.c19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx2() local
25 q = (u8 *)ptrs[disks-1]; in raid6_2data_recov_avx2()
43 ptrs[disks-1] = q; in raid6_2data_recov_avx2()
57 asm volatile("vmovdqa %0, %%ymm1" : : "m" (q[0])); in raid6_2data_recov_avx2()
130 q += 64; in raid6_2data_recov_avx2()
177 q += 32; in raid6_2data_recov_avx2()
189 u8 *p, *q, *dq; in raid6_datap_recov_avx2() local
194 q = (u8 *)ptrs[disks-1]; in raid6_datap_recov_avx2()
206 ptrs[disks-1] = q; in raid6_datap_recov_avx2()
265 q += 64; in raid6_datap_recov_avx2()
[all …]
A Dloongarch_simd.c36 u8 *p, *q; in raid6_lsx_gen_syndrome() local
41 q = dptr[z0+2]; /* RS syndrome */ in raid6_lsx_gen_syndrome()
118 u8 *p, *q; in raid6_lsx_xor_syndrome() local
123 q = dptr[disks-1]; /* RS syndrome */ in raid6_lsx_xor_syndrome()
237 "+m"(q[d+NSIZE*0]), "+m"(q[d+NSIZE*1]), in raid6_lsx_xor_syndrome()
238 "+m"(q[d+NSIZE*2]), "+m"(q[d+NSIZE*3]) in raid6_lsx_xor_syndrome()
267 u8 *p, *q; in raid6_lasx_gen_syndrome() local
272 q = dptr[z0+2]; /* RS syndrome */ in raid6_lasx_gen_syndrome()
327 u8 *p, *q; in raid6_lasx_xor_syndrome() local
332 q = dptr[disks-1]; /* RS syndrome */ in raid6_lasx_xor_syndrome()
[all …]
A Drecov_avx512.c25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_avx512() local
31 q = (u8 *)ptrs[disks-1]; in raid6_2data_recov_avx512()
52 ptrs[disks-1] = q; in raid6_2data_recov_avx512()
75 : "m" (q[0]), "m" (q[64]), "m" (p[0]), in raid6_2data_recov_avx512()
155 q += 128; in raid6_2data_recov_avx512()
216 q += 64; in raid6_2data_recov_avx512()
228 u8 *p, *q, *dq; in raid6_datap_recov_avx512() local
248 ptrs[disks-1] = q; in raid6_datap_recov_avx512()
265 "m" (q[64])); in raid6_datap_recov_avx512()
319 q += 128; in raid6_datap_recov_avx512()
[all …]
A Drecov_ssse3.c19 u8 *p, *q, *dp, *dq; in raid6_2data_recov_ssse3() local
27 q = (u8 *)ptrs[disks-1]; in raid6_2data_recov_ssse3()
45 ptrs[disks-1] = q; in raid6_2data_recov_ssse3()
67 asm volatile("movdqa %0,%%xmm1" : : "m" (q[0])); in raid6_2data_recov_ssse3()
134 q += 32; in raid6_2data_recov_ssse3()
181 q += 16; in raid6_2data_recov_ssse3()
194 u8 *p, *q, *dq; in raid6_datap_recov_ssse3() local
201 q = (u8 *)ptrs[disks-1]; in raid6_datap_recov_ssse3()
213 ptrs[disks-1] = q; in raid6_datap_recov_ssse3()
279 q += 32; in raid6_datap_recov_ssse3()
[all …]
A Drecov_rvv.c80 [qx]"r"(q), in __raid6_2data_recov_rvv()
90 q += 16; in __raid6_2data_recov_rvv()
138 [vx]"r"(q), in __raid6_datap_recov_rvv()
147 q += 16; in __raid6_datap_recov_rvv()
155 u8 *p, *q, *dp, *dq; in raid6_2data_recov_rvv() local
160 q = (u8 *)ptrs[disks - 1]; in raid6_2data_recov_rvv()
180 ptrs[disks - 1] = q; in raid6_2data_recov_rvv()
195 u8 *p, *q, *dq; in raid6_datap_recov_rvv() local
199 q = (u8 *)ptrs[disks - 1]; in raid6_datap_recov_rvv()
213 ptrs[disks - 1] = q; in raid6_datap_recov_rvv()
[all …]
A Drecov.c22 u8 *p, *q, *dp, *dq; in raid6_2data_recov_intx1() local
28 q = (u8 *)ptrs[disks-1]; in raid6_2data_recov_intx1()
46 ptrs[disks-1] = q; in raid6_2data_recov_intx1()
55 qx = qmul[*q ^ *dq]; in raid6_2data_recov_intx1()
58 p++; q++; in raid6_2data_recov_intx1()
66 u8 *p, *q, *dq; in raid6_datap_recov_intx1() local
70 q = (u8 *)ptrs[disks-1]; in raid6_datap_recov_intx1()
82 ptrs[disks-1] = q; in raid6_datap_recov_intx1()
89 *p++ ^= *dq = qmul[*q ^ *dq]; in raid6_datap_recov_intx1()
90 q++; dq++; in raid6_datap_recov_intx1()
A Drecov_s390xc.c25 u8 *p, *q, *dp, *dq; in raid6_2data_recov_s390xc() local
31 q = (u8 *)ptrs[disks-1]; in raid6_2data_recov_s390xc()
49 ptrs[disks-1] = q; in raid6_2data_recov_s390xc()
58 xor_block(dq, q); in raid6_2data_recov_s390xc()
63 q += 256; in raid6_2data_recov_s390xc()
74 u8 *p, *q, *dq; in raid6_datap_recov_s390xc() local
79 q = (u8 *)ptrs[disks-1]; in raid6_datap_recov_s390xc()
91 ptrs[disks-1] = q; in raid6_datap_recov_s390xc()
98 xor_block(dq, q); in raid6_datap_recov_s390xc()
103 q += 256; in raid6_datap_recov_s390xc()
A Drecov_neon.c26 u8 *p, *q, *dp, *dq; in raid6_2data_recov_neon() local
31 q = (u8 *)ptrs[disks - 1]; in raid6_2data_recov_neon()
51 ptrs[disks - 1] = q; in raid6_2data_recov_neon()
59 __raid6_2data_recov_neon(bytes, p, q, dp, dq, pbmul, qmul); in raid6_2data_recov_neon()
66 u8 *p, *q, *dq; in raid6_datap_recov_neon() local
70 q = (u8 *)ptrs[disks - 1]; in raid6_datap_recov_neon()
84 ptrs[disks - 1] = q; in raid6_datap_recov_neon()
90 __raid6_datap_recov_neon(bytes, p, q, dq, qmul); in raid6_datap_recov_neon()
A Dmmx.c38 u8 *p, *q; in raid6_mmx1_gen_syndrome() local
43 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx1_gen_syndrome()
65 asm volatile("movq %%mm4,%0" : "=m" (q[d])); in raid6_mmx1_gen_syndrome()
86 u8 *p, *q; in raid6_mmx2_gen_syndrome() local
91 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
124 asm volatile("movq %%mm4,%0" : "=m" (q[d])); in raid6_mmx2_gen_syndrome()
125 asm volatile("movq %%mm6,%0" : "=m" (q[d+8])); in raid6_mmx2_gen_syndrome()
A Dsse1.c43 u8 *p, *q; in raid6_sse11_gen_syndrome() local
48 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse11_gen_syndrome()
81 asm volatile("movntq %%mm4,%0" : "=m" (q[d])); in raid6_sse11_gen_syndrome()
102 u8 *p, *q; in raid6_sse12_gen_syndrome() local
107 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse12_gen_syndrome()
143 asm volatile("movntq %%mm4,%0" : "=m" (q[d])); in raid6_sse12_gen_syndrome()
144 asm volatile("movntq %%mm6,%0" : "=m" (q[d+8])); in raid6_sse12_gen_syndrome()
A Drecov_neon_inner.c28 void __raid6_2data_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dp, in __raid6_2data_recov_neon() argument
54 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); in __raid6_2data_recov_neon()
72 q += 16; in __raid6_2data_recov_neon()
78 void __raid6_datap_recov_neon(int bytes, uint8_t *p, uint8_t *q, uint8_t *dq, in __raid6_datap_recov_neon() argument
95 vx = veorq_u8(vld1q_u8(q), vld1q_u8(dq)); in __raid6_datap_recov_neon()
108 q += 16; in __raid6_datap_recov_neon()
/lib/math/
A Dcordic.c55 coord.q = 0; in cordic_calc_iq()
73 valtmp = coord.i - (coord.q >> iter); in cordic_calc_iq()
74 coord.q += (coord.i >> iter); in cordic_calc_iq()
77 valtmp = coord.i + (coord.q >> iter); in cordic_calc_iq()
78 coord.q -= (coord.i >> iter); in cordic_calc_iq()
85 coord.q *= signx; in cordic_calc_iq()
/lib/zlib_inflate/
A Dinflate.h115 #define REVERSE(q) \ argument
116 ((((q) >> 24) & 0xff) + (((q) >> 8) & 0xff00) + \
117 (((q) & 0xff00) << 8) + (((q) & 0xff) << 24))
/lib/crypto/mpi/
A Dmpih-div.c248 mpi_limb_t q; in mpihelp_divrem() local
260 q = ~(mpi_limb_t) 0; in mpihelp_divrem()
266 qp[i] = q; in mpihelp_divrem()
273 umul_ppmm(n1, n0, d0, q); in mpihelp_divrem()
280 q--; in mpihelp_divrem()
287 qp[i] = q; in mpihelp_divrem()
315 mpi_limb_t q; in mpihelp_divrem() local
331 q = ~(mpi_limb_t) 0; in mpihelp_divrem()
341 q--; in mpihelp_divrem()
357 q--; in mpihelp_divrem()
[all …]
A Dlonglong.h144 #define udiv_qrnnd(q, r, n1, n0, d) \ argument
146 : "=r" ((USItype)(q)), \
162 #define udiv_qrnnd(q, r, n1, n0, d) \ argument
289 : "=g" ((USItype)(q)), \
423 : "=a" (q), \
543 : "=d" ((USItype)(q)), \
551 : "=d" ((USItype)(q)), \
992 (q) = __q; \
1047 : "=r" ((USItype)(q)), \
1132 : "=&r" ((USItype)(q)), \
[all …]
/lib/crypto/arm/
A Dsha256-ce.S40 vadd.u32 ta\ev, q\s0, k\ev
45 sha256su0.32 q\s0, q\s1
47 sha256su1.32 q\s0, q\s2, q\s3

Completed in 33 milliseconds

12