Home
last modified time | relevance | path

Searched refs:dptr (Results 1 – 11 of 11) sorted by relevance

/lib/raid6/
Davx2.c38 u8 **dptr = (u8 **)ptrs; in raid6_avx21_gen_syndrome() local
43 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
44 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
53 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
54 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
56 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
65 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
87 u8 **dptr = (u8 **)ptrs; in raid6_avx21_xor_syndrome() local
[all …]
Dsse2.c38 u8 **dptr = (u8 **)ptrs; in raid6_sse21_gen_syndrome() local
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()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
66 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
90 u8 **dptr = (u8 **)ptrs; in raid6_sse21_xor_syndrome() local
[all …]
Davx512.c46 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_gen_syndrome() local
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()
80 : "m" (dptr[z][d])); in raid6_avx5121_gen_syndrome()
104 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_xor_syndrome() local
109 p = dptr[disks-2]; /* XOR parity */ in raid6_avx5121_xor_syndrome()
110 q = dptr[disks-1]; /* RS syndrome */ in raid6_avx5121_xor_syndrome()
122 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
135 : "m" (dptr[z][d])); in raid6_avx5121_xor_syndrome()
[all …]
Dsse1.c42 u8 **dptr = (u8 **)ptrs; in raid6_sse11_gen_syndrome() local
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()
62 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
70 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
101 u8 **dptr = (u8 **)ptrs; in raid6_sse12_gen_syndrome() local
[all …]
Dmmx.c37 u8 **dptr = (u8 **)ptrs; in raid6_mmx1_gen_syndrome() local
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()
54 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_mmx1_gen_syndrome()
85 u8 **dptr = (u8 **)ptrs; in raid6_mmx2_gen_syndrome() local
90 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
91 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
100 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx2_gen_syndrome()
101 asm volatile("movq %0,%%mm3" : : "m" (dptr[z0][d+8])); in raid6_mmx2_gen_syndrome()
[all …]
Ds390vx.uc86 u8 **dptr, *p, *q;
92 dptr = (u8 **) ptrs;
94 p = dptr[z0 + 1]; /* XOR parity */
95 q = dptr[z0 + 2]; /* RS syndrome */
98 LOAD_DATA(0,&dptr[z0][d]);
105 LOAD_DATA(16,&dptr[z][d]);
119 u8 **dptr, *p, *q;
122 dptr = (u8 **) ptrs;
124 p = dptr[disks - 2]; /* XOR parity */
125 q = dptr[disks - 1]; /* RS syndrome */
[all …]
Dneon.uc58 uint8_t **dptr = (uint8_t **)ptrs;
66 p = dptr[z0+1]; /* XOR parity */
67 q = dptr[z0+2]; /* RS syndrome */
70 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
72 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
89 uint8_t **dptr = (uint8_t **)ptrs;
97 p = dptr[disks-2]; /* XOR parity */
98 q = dptr[disks-1]; /* RS syndrome */
101 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
106 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
Dint.uc84 u8 **dptr = (u8 **)ptrs;
91 p = dptr[z0+1]; /* XOR parity */
92 q = dptr[z0+2]; /* RS syndrome */
95 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
97 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
113 u8 **dptr = (u8 **)ptrs;
120 p = dptr[disks-2]; /* XOR parity */
121 q = dptr[disks-1]; /* RS syndrome */
125 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
127 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
Dvpermxor.uc46 u8 **dptr = (u8 **)ptrs;
52 p = dptr[z0+1]; /* XOR parity */
53 q = dptr[z0+2]; /* RS syndrome */
56 wp$$ = wq$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
59 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
Daltivec.uc73 u8 **dptr = (u8 **)ptrs;
81 p = dptr[z0+1]; /* XOR parity */
82 q = dptr[z0+2]; /* RS syndrome */
85 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
87 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
/lib/
Dearlycpio.c64 const char *p, *dptr, *nptr; in find_cpio_data() local
111 dptr = PTR_ALIGN(p + ch[C_NAMESIZE], 4); in find_cpio_data()
112 nptr = PTR_ALIGN(dptr + ch[C_FILESIZE], 4); in find_cpio_data()
114 if (nptr > p + len || dptr < p || nptr < dptr) in find_cpio_data()
131 cd.data = (void *)dptr; in find_cpio_data()