Home
last modified time | relevance | path

Searched refs:z0 (Results 1 – 25 of 31) sorted by relevance

12

/linux-6.12.1/lib/raid6/
Davx2.c38 int d, z, z0; in raid6_avx21_gen_syndrome() local
40 z0 = disks - 3; /* Highest data disk */ in raid6_avx21_gen_syndrome()
41 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
42 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
50 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
51 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
54 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
55 for (z = z0-2; z >= 0; z--) { in raid6_avx21_gen_syndrome()
87 int d, z, z0; in raid6_avx21_xor_syndrome() local
[all …]
Dsse2.c40 int d, z, z0; in raid6_sse21_gen_syndrome() local
42 z0 = disks - 3; /* Highest data disk */ in raid6_sse21_gen_syndrome()
43 p = dptr[z0+1]; /* XOR parity */ in raid6_sse21_gen_syndrome()
44 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse21_gen_syndrome()
53 asm volatile("movdqa %0,%%xmm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse21_gen_syndrome()
54 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
56 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
57 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse21_gen_syndrome()
92 int d, z, z0; in raid6_sse21_xor_syndrome() local
[all …]
Davx512.c48 int d, z, z0; in raid6_avx5121_gen_syndrome() local
50 z0 = disks - 3; /* Highest data disk */ in raid6_avx5121_gen_syndrome()
51 p = dptr[z0+1]; /* XOR parity */ in raid6_avx5121_gen_syndrome()
52 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx5121_gen_syndrome()
68 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
69 for (z = z0-2; z >= 0; z--) { in raid6_avx5121_gen_syndrome()
106 int d, z, z0; in raid6_avx5121_xor_syndrome() local
108 z0 = stop; /* P/Q right side optimization */ in raid6_avx5121_xor_syndrome()
122 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
124 for (z = z0-1 ; z >= start ; z--) { in raid6_avx5121_xor_syndrome()
[all …]
Dloongarch_simd.c37 int d, z, z0; in raid6_lsx_gen_syndrome() local
39 z0 = disks - 3; /* Highest data disk */ in raid6_lsx_gen_syndrome()
40 p = dptr[z0+1]; /* XOR parity */ in raid6_lsx_gen_syndrome()
41 q = dptr[z0+2]; /* RS syndrome */ in raid6_lsx_gen_syndrome()
54 asm volatile("vld $vr0, %0" : : "m"(dptr[z0][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
55 asm volatile("vld $vr1, %0" : : "m"(dptr[z0][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
56 asm volatile("vld $vr2, %0" : : "m"(dptr[z0][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
57 asm volatile("vld $vr3, %0" : : "m"(dptr[z0][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
62 for (z = z0-1; z >= 0; z--) { in raid6_lsx_gen_syndrome()
119 int d, z, z0; in raid6_lsx_xor_syndrome() local
[all …]
Dsse1.c44 int d, z, z0; in raid6_sse11_gen_syndrome() local
46 z0 = disks - 3; /* Highest data disk */ in raid6_sse11_gen_syndrome()
47 p = dptr[z0+1]; /* XOR parity */ in raid6_sse11_gen_syndrome()
48 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse11_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse11_gen_syndrome()
57 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse11_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
60 asm volatile("movq %0,%%mm6" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
61 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse11_gen_syndrome()
103 int d, z, z0; in raid6_sse12_gen_syndrome() local
[all …]
Dmmx.c39 int d, z, z0; in raid6_mmx1_gen_syndrome() local
41 z0 = disks - 3; /* Highest data disk */ in raid6_mmx1_gen_syndrome()
42 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx1_gen_syndrome()
43 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx1_gen_syndrome()
51 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx1_gen_syndrome()
53 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx1_gen_syndrome()
87 int d, z, z0; in raid6_mmx2_gen_syndrome() local
89 z0 = disks - 3; /* Highest data disk */ in raid6_mmx2_gen_syndrome()
90 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
91 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
[all …]
Ds390vx.uc50 int d, z, z0;
56 z0 = disks - 3; /* Highest data disk */
57 p = dptr[z0 + 1]; /* XOR parity */
58 q = dptr[z0 + 2]; /* RS syndrome */
61 LOAD_DATA(0,&dptr[z0][d]);
63 for (z = z0 - 1; z >= 0; z--) {
83 int d, z, z0;
86 z0 = stop; /* P/Q right side optimization */
95 LOAD_DATA(0,&dptr[z0][d]);
97 for (z = z0 - 1; z >= start; z--) {
Dint.uc79 int d, z, z0;
83 z0 = disks - 3; /* Highest data disk */
84 p = dptr[z0+1]; /* XOR parity */
85 q = dptr[z0+2]; /* RS syndrome */
88 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
89 for ( z = z0-1 ; z >= 0 ; z-- ) {
108 int d, z, z0;
112 z0 = stop; /* P/Q right side optimization */
118 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
119 for ( z = z0-1 ; z >= start ; z-- ) {
Dneon.uc61 int d, z, z0;
66 z0 = disks - 3; /* Highest data disk */
67 p = dptr[z0+1]; /* XOR parity */
68 q = dptr[z0+2]; /* RS syndrome */
71 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
72 for ( z = z0-1 ; z >= 0 ; z-- ) {
92 int d, z, z0;
97 z0 = stop; /* P/Q right side optimization */
102 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
106 for ( z = z0-1 ; z >= start ; z-- ) {
Dvpermxor.uc48 int d, z, z0;
51 z0 = disks - 3; /* Highest data disk */
52 p = dptr[z0+1]; /* XOR parity */
53 q = dptr[z0+2]; /* RS syndrome */
56 wp$$ = wq$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
58 for (z = z0-1; z>=0; z--) {
Daltivec.uc75 int d, z, z0;
80 z0 = disks - 3; /* Highest data disk */
81 p = dptr[z0+1]; /* XOR parity */
82 q = dptr[z0+2]; /* RS syndrome */
85 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
86 for ( z = z0-1 ; z >= 0 ; z-- ) {
/linux-6.12.1/arch/arm/nwfpe/
Dsoftfloat-macros107 bits64 z0, z1;
112 z0 = a0;
116 z0 = a0>>count;
125 z0 = 0;
128 *z0Ptr = z0;
145 bits64 z0, z1;
150 z0 = a0;
154 z0 = a0>>count;
158 z0 = 0;
161 *z0Ptr = z0;
[all …]
/linux-6.12.1/drivers/isdn/mISDN/
Ddsp_biquad.h42 int32_t z0; in biquad2() local
44 z0 = sample * bq->gain + bq->z1 * bq->a1 + bq->z2 * bq->a2; in biquad2()
45 y = z0 + bq->z1 * bq->b1 + bq->z2 * bq->b2; in biquad2()
48 bq->z1 = z0 >> 15; in biquad2()
/linux-6.12.1/arch/x86/crypto/
Daria-gfni-avx512-asm_64.S425 z0, z1, z2, z3, \ argument
430 z0, rk, round); \
436 z0, z1, z2, z3, \
439 aria_diff_m(x0, x1, x2, x3, z0, z1, z2, z3); \
440 aria_diff_m(x4, x5, x6, x7, z0, z1, z2, z3); \
441 aria_diff_m(y0, y1, y2, y3, z0, z1, z2, z3); \
442 aria_diff_m(y4, y5, y6, y7, z0, z1, z2, z3); \
465 z0, z1, z2, z3, \ argument
470 z0, rk, round); \
476 z0, z1, z2, z3, \
[all …]
Dcurve25519-x86_64.c1060 u64 *z0; in montgomery_ladder() local
1071 z0 = p03 + (u32)4U; in montgomery_ladder()
1076 z0[0U] = (u64)0U; in montgomery_ladder()
1077 z0[1U] = (u64)0U; in montgomery_ladder()
1078 z0[2U] = (u64)0U; in montgomery_ladder()
1079 z0[3U] = (u64)0U; in montgomery_ladder()
/linux-6.12.1/Documentation/input/devices/
Dalps.rst114 byte 5: 0 z6 z5 z4 z3 z2 z1 z0
126 byte 5: 0 z6 z5 z4 z3 z2 z1 z0
147 byte 8: 0 z6 z5 z4 z3 z2 z1 z0
168 byte 5: 0 z6 z5 z4 z3 z2 z1 z0
196 byte 4: 0 z6 z5 z4 z3 z2 z1 z0
212 byte 5: 0 z6 z5 z4 z3 z2 z1 z0
260 byte 5: 0 z6 z5 z4 z3 z2 z1 z0
290 byte 5: z7 z6 z5 z4 z3 z2 z1 z0
/linux-6.12.1/arch/arm/boot/dts/marvell/
Dkirkwood-rd88f6281-z0.dts17 …compatible = "marvell,rd88f6281-z0", "marvell,rd88f6281","marvell,kirkwood-88f6281", "marvell,kirk…
/linux-6.12.1/Documentation/devicetree/bindings/thermal/
Damazon,al-thermal.txt19 thermal-z0 {
/linux-6.12.1/arch/sh/kernel/cpu/sh4/
Dsoftfloat.c685 bits64 z0, zMiddleA, zMiddleB, z1; in mul64To128() local
694 z0 = ((bits64) aHigh) * bHigh; in mul64To128()
696 z0 += (((bits64) (zMiddleA < zMiddleB)) << 32) + (zMiddleA >> 32); in mul64To128()
699 z0 += (z1 < zMiddleA); in mul64To128()
701 *z0Ptr = z0; in mul64To128()
/linux-6.12.1/scripts/kconfig/
Dlexer.l94 n [A-Za-z0-9_-]
/linux-6.12.1/scripts/
Dverify_builtin_ranges.awk202 ARGIND >= 4 && map_is_lld && NF == 5 && $5 ~ /^[A-Za-z_][A-Za-z0-9_]*$/ {
Dgenerate_builtin_ranges.awk159 ARGIND == 2 && map_is_lld && sect && !anchor && NF == 5 && $5 ~ /^[_A-Za-z][_A-Za-z0-9]*$/ {
/linux-6.12.1/tools/testing/selftests/arm64/fp/
Dfp-ptrace-asm.S85 ldr z0, [x7, #0, MUL VL]
212 str z0, [x7, #0, MUL VL]
/linux-6.12.1/scripts/genksyms/
Dlex.l28 IDENT [A-Za-z_\$][A-Za-z0-9_\$]*
/linux-6.12.1/tools/testing/selftests/arm64/abi/
Dsyscall-abi-asm.S156 ldr z0, [x2, #0, MUL VL]
289 str z0, [x2, #0, MUL VL]

12