| /linux-4.19.296/lib/raid6/ |
| D | avx2.c | 44 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()
93 u8 **dptr = (u8 **)ptrs; in raid6_avx21_xor_syndrome() local
[all …]
|
| D | sse2.c | 43 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 …]
|
| D | avx512.c | 51 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 …]
|
| D | sse1.c | 47 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 …]
|
| D | mmx.c | 42 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 …]
|
| D | s390vx.uc | 86 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 …]
|
| D | neon.uc | 58 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]);
|
| D | int.uc | 84 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];
|
| D | vpermxor.uc | 46 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];
|
| D | altivec.uc | 73 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];
|
| /linux-4.19.296/include/linux/netfilter/ |
| D | nf_conntrack_sip.h | 46 const char **dptr, unsigned int *datalen,
50 const char **dptr, unsigned int *datalen,
70 const char *dptr, const char *limit,
115 const char **dptr,
124 const char **dptr,
133 const char **dptr,
143 const char **dptr,
152 const char **dptr,
160 const char **dptr,
170 int ct_sip_parse_request(const struct nf_conn *ct, const char *dptr,
[all …]
|
| /linux-4.19.296/lib/ |
| D | earlycpio.c | 72 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()
|
| /linux-4.19.296/include/linux/ |
| D | nvme.h | 641 union nvme_data_ptr dptr; member
652 union nvme_data_ptr dptr; member
693 union nvme_data_ptr dptr; member
720 union nvme_data_ptr dptr; member
829 union nvme_data_ptr dptr; member
844 union nvme_data_ptr dptr; member
912 union nvme_data_ptr dptr; member
934 union nvme_data_ptr dptr; member
951 union nvme_data_ptr dptr; member
1039 union nvme_data_ptr dptr; member
|
| /linux-4.19.296/fs/xfs/ |
| D | xfs_log.c | 1889 char *dptr; in xlog_sync() local
1902 dptr = (char *)&iclog->ic_header + count; in xlog_sync()
1904 uint32_t cycle = be32_to_cpu(*(__be32 *)dptr); in xlog_sync()
1907 *(__be32 *)dptr = cpu_to_be32(cycle); in xlog_sync()
1909 dptr += BBSIZE; in xlog_sync()
|
| /linux-4.19.296/fs/gfs2/ |
| D | ops_fstype.c | 442 static int gfs2_lookup_root(struct super_block *sb, struct dentry **dptr, in gfs2_lookup_root() argument
460 *dptr = dentry; in gfs2_lookup_root()
|