Home
last modified time | relevance | path

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

/lib/raid6/
Dsse2.c43 u8 **dptr = (u8 **)ptrs; in raid6_sse21_gen_syndrome() local
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()
63 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
71 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
95 u8 **dptr = (u8 **)ptrs; in raid6_sse21_xor_syndrome() local
[all …]
Davx2.c44 u8 **dptr = (u8 **)ptrs; in raid6_avx21_gen_syndrome() local
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()
64 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
71 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
103 u8 **dptr = (u8 **)ptrs; in raid6_avx22_gen_syndrome() local
[all …]
Davx512.c51 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_gen_syndrome() local
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()
85 : "m" (dptr[z][d])); in raid6_avx5121_gen_syndrome()
109 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_xor_syndrome() local
114 p = dptr[disks-2]; /* XOR parity */ in raid6_avx5121_xor_syndrome()
115 q = dptr[disks-1]; /* RS syndrome */ in raid6_avx5121_xor_syndrome()
127 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
140 : "m" (dptr[z][d])); in raid6_avx5121_xor_syndrome()
[all …]
Dsse1.c47 u8 **dptr = (u8 **)ptrs; in raid6_sse11_gen_syndrome() local
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()
67 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
75 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
106 u8 **dptr = (u8 **)ptrs; in raid6_sse12_gen_syndrome() local
[all …]
Dmmx.c42 u8 **dptr = (u8 **)ptrs; in raid6_mmx1_gen_syndrome() local
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()
59 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_mmx1_gen_syndrome()
90 u8 **dptr = (u8 **)ptrs; in raid6_mmx2_gen_syndrome() local
95 p = dptr[z0+1]; /* XOR parity */ in raid6_mmx2_gen_syndrome()
96 q = dptr[z0+2]; /* RS syndrome */ in raid6_mmx2_gen_syndrome()
105 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx2_gen_syndrome()
106 asm volatile("movq %0,%%mm3" : : "m" (dptr[z0][d+8])); in raid6_mmx2_gen_syndrome()
[all …]
Ds390vx.uc83 u8 **dptr, *p, *q;
89 dptr = (u8 **) ptrs;
91 p = dptr[z0 + 1]; /* XOR parity */
92 q = dptr[z0 + 2]; /* RS syndrome */
95 LOAD_DATA(0,$#,&dptr[z0][d]);
102 LOAD_DATA(16,$#,&dptr[z][d]);
116 u8 **dptr, *p, *q;
119 dptr = (u8 **) ptrs;
121 p = dptr[disks - 2]; /* XOR parity */
122 q = dptr[disks - 1]; /* RS syndrome */
[all …]
Dneon.uc55 uint8_t **dptr = (uint8_t **)ptrs;
63 p = dptr[z0+1]; /* XOR parity */
64 q = dptr[z0+2]; /* RS syndrome */
67 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
69 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
86 uint8_t **dptr = (uint8_t **)ptrs;
94 p = dptr[disks-2]; /* XOR parity */
95 q = dptr[disks-1]; /* RS syndrome */
98 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
103 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];
Dtilegx.uc52 u8 **dptr = (u8 **)ptrs;
61 p = (u64 *)dptr[z0+1]; /* XOR parity */
62 q = (u64 *)dptr[z0+2]; /* RS syndrome */
64 z0ptr = (u64 *)&dptr[z0][0];
68 wd$$ = *(u64 *)&dptr[z][d+$$*NSIZE];
Daltivec.uc70 u8 **dptr = (u8 **)ptrs;
78 p = dptr[z0+1]; /* XOR parity */
79 q = dptr[z0+2]; /* RS syndrome */
82 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
84 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
/lib/
Dearlycpio.c72 const char *p, *dptr, *nptr; in find_cpio_data() local
119 dptr = PTR_ALIGN(p + ch[C_NAMESIZE], 4); in find_cpio_data()
120 nptr = PTR_ALIGN(dptr + ch[C_FILESIZE], 4); in find_cpio_data()
122 if (nptr > p + len || dptr < p || nptr < dptr) in find_cpio_data()
139 cd.data = (void *)dptr; in find_cpio_data()