Home
last modified time | relevance | path

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

12

/Linux-v6.6/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 …]
Dint.uc86 int d, z, z0;
90 z0 = disks - 3; /* Highest data disk */
91 p = dptr[z0+1]; /* XOR parity */
92 q = dptr[z0+2]; /* RS syndrome */
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
96 for ( z = z0-1 ; z >= 0 ; z-- ) {
115 int d, z, z0;
119 z0 = stop; /* P/Q right side optimization */
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
126 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-- ) {
Ds390vx.uc86 int d, z, z0;
92 z0 = disks - 3; /* Highest data disk */
93 p = dptr[z0 + 1]; /* XOR parity */
94 q = dptr[z0 + 2]; /* RS syndrome */
97 LOAD_DATA(0,&dptr[z0][d]);
99 for (z = z0 - 1; z >= 0; z--) {
119 int d, z, z0;
122 z0 = stop; /* P/Q right side optimization */
131 LOAD_DATA(0,&dptr[z0][d]);
133 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-v6.6/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-v6.6/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-v6.6/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-v6.6/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-v6.6/arch/arm/boot/dts/marvell/
Dkirkwood-rd88f6281-z0.dts17 …compatible = "marvell,rd88f6281-z0", "marvell,rd88f6281","marvell,kirkwood-88f6281", "marvell,kirk…
DMakefile153 kirkwood-rd88f6281-z0.dtb \
/Linux-v6.6/Documentation/devicetree/bindings/thermal/
Damazon,al-thermal.txt19 thermal-z0 {
/Linux-v6.6/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-v6.6/scripts/kconfig/
Dlexer.l84 n [A-Za-z0-9_-]
/Linux-v6.6/scripts/genksyms/
Dlex.l28 IDENT [A-Za-z_\$][A-Za-z0-9_\$]*
/Linux-v6.6/tools/testing/selftests/arm64/abi/
Dsyscall-abi-asm.S156 ldr z0, [x2, #0, MUL VL]
289 str z0, [x2, #0, MUL VL]
/Linux-v6.6/drivers/scsi/aic7xxx/aicasm/
Daicasm_scan.l69 PATH ([/]*[-A-Za-z0-9_.])+
/Linux-v6.6/arch/arm64/boot/dts/rockchip/
Dpx30-evb.dts408 "0", /* z0 */

12