| /linux-4.19.296/lib/raid6/ |
| D | avx2.c | 46 int d, z, z0; in raid6_avx21_gen_syndrome() local
48 z0 = disks - 3; /* Highest data disk */ in raid6_avx21_gen_syndrome()
49 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
50 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
59 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
60 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
62 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
63 for (z = z0-2; z >= 0; z--) { in raid6_avx21_gen_syndrome()
95 int d, z, z0; in raid6_avx21_xor_syndrome() local
[all …]
|
| D | sse2.c | 45 int d, z, z0; in raid6_sse21_gen_syndrome() local
47 z0 = disks - 3; /* Highest data disk */ in raid6_sse21_gen_syndrome()
48 p = dptr[z0+1]; /* XOR parity */ in raid6_sse21_gen_syndrome()
49 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse21_gen_syndrome()
57 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse21_gen_syndrome()
58 asm volatile("movdqa %0,%%xmm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse21_gen_syndrome()
59 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
61 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
62 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse21_gen_syndrome()
97 int d, z, z0; in raid6_sse21_xor_syndrome() local
[all …]
|
| D | avx512.c | 53 int d, z, z0; in raid6_avx5121_gen_syndrome() local
55 z0 = disks - 3; /* Highest data disk */ in raid6_avx5121_gen_syndrome()
56 p = dptr[z0+1]; /* XOR parity */ in raid6_avx5121_gen_syndrome()
57 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx5121_gen_syndrome()
73 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
74 for (z = z0-2; z >= 0; z--) { in raid6_avx5121_gen_syndrome()
111 int d, z, z0; in raid6_avx5121_xor_syndrome() local
113 z0 = stop; /* P/Q right side optimization */ in raid6_avx5121_xor_syndrome()
127 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
129 for (z = z0-1 ; z >= start ; z--) { in raid6_avx5121_xor_syndrome()
[all …]
|
| D | sse1.c | 49 int d, z, z0; in raid6_sse11_gen_syndrome() local
51 z0 = disks - 3; /* Highest data disk */ in raid6_sse11_gen_syndrome()
52 p = dptr[z0+1]; /* XOR parity */ in raid6_sse11_gen_syndrome()
53 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse11_gen_syndrome()
61 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse11_gen_syndrome()
62 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse11_gen_syndrome()
63 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
65 asm volatile("movq %0,%%mm6" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
66 for ( z = z0-2 ; z >= 0 ; z-- ) { in raid6_sse11_gen_syndrome()
108 int d, z, z0; in raid6_sse12_gen_syndrome() local
[all …]
|
| D | mmx.c | 44 int d, z, z0; in raid6_mmx1_gen_syndrome() local
46 z0 = disks - 3; /* Highest data disk */ in raid6_mmx1_gen_syndrome()
47 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx1_gen_syndrome()
48 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx1_gen_syndrome()
56 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx1_gen_syndrome()
58 for ( z = z0-1 ; z >= 0 ; z-- ) { in raid6_mmx1_gen_syndrome()
92 int d, z, z0; in raid6_mmx2_gen_syndrome() local
94 z0 = disks - 3; /* Highest data disk */ in raid6_mmx2_gen_syndrome()
95 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
96 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
[all …]
|
| D | s390vx.uc | 87 int d, z, z0;
93 z0 = disks - 3; /* Highest data disk */
94 p = dptr[z0 + 1]; /* XOR parity */
95 q = dptr[z0 + 2]; /* RS syndrome */
98 LOAD_DATA(0,&dptr[z0][d]);
100 for (z = z0 - 1; z >= 0; z--) {
120 int d, z, z0;
123 z0 = stop; /* P/Q right side optimization */
132 LOAD_DATA(0,&dptr[z0][d]);
134 for (z = z0 - 1; z >= start; z--) {
|
| D | neon.uc | 60 int d, z, z0;
65 z0 = disks - 3; /* Highest data disk */
66 p = dptr[z0+1]; /* XOR parity */
67 q = dptr[z0+2]; /* RS syndrome */
70 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
71 for ( z = z0-1 ; z >= 0 ; z-- ) {
91 int d, z, z0;
96 z0 = stop; /* P/Q right side optimization */
101 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
105 for ( z = z0-1 ; z >= start ; z-- ) {
|
| D | int.uc | 86 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-- ) {
|
| D | vpermxor.uc | 48 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--) {
|
| D | altivec.uc | 75 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-4.19.296/drivers/isdn/mISDN/ |
| D | dsp_biquad.h | 56 int32_t z0; in biquad2() local
58 z0 = sample * bq->gain + bq->z1 * bq->a1 + bq->z2 * bq->a2; in biquad2()
59 y = z0 + bq->z1 * bq->b1 + bq->z2 * bq->b2; in biquad2()
62 bq->z1 = z0 >> 15; in biquad2()
|
| /linux-4.19.296/ |
| D | MAINTAINERS | 8447 N: [^a-z0-9]ps3
|