Home
last modified time | relevance | path

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

123

/linux/net/netrom/
A Dnr_subr.c160 *dptr++ = 0; in nr_write_internal()
161 *dptr++ = 0; in nr_write_internal()
193 *dptr++ = 0; in nr_write_internal()
194 *dptr++ = 0; in nr_write_internal()
201 *dptr++ = 0; in nr_write_internal()
202 *dptr++ = nr->vr; in nr_write_internal()
243 *dptr++ = 0; in __nr_transmit_reply()
244 *dptr++ = 0; in __nr_transmit_reply()
250 *dptr++ = 0; in __nr_transmit_reply()
251 *dptr++ = 0; in __nr_transmit_reply()
[all …]
A Dnr_out.c188 unsigned char *dptr; in nr_transmit_buffer() local
193 dptr = skb_push(skb, NR_NETWORK_LEN); in nr_transmit_buffer()
196 dptr[6] &= ~AX25_CBIT; in nr_transmit_buffer()
197 dptr[6] &= ~AX25_EBIT; in nr_transmit_buffer()
198 dptr[6] |= AX25_SSSID_SPARE; in nr_transmit_buffer()
199 dptr += AX25_ADDR_LEN; in nr_transmit_buffer()
201 memcpy(dptr, &nr->dest_addr, AX25_ADDR_LEN); in nr_transmit_buffer()
202 dptr[6] &= ~AX25_CBIT; in nr_transmit_buffer()
203 dptr[6] |= AX25_EBIT; in nr_transmit_buffer()
204 dptr[6] |= AX25_SSSID_SPARE; in nr_transmit_buffer()
[all …]
/linux/net/netfilter/
A Dnf_conntrack_sip.c135 if (dptr >= limit || *dptr != ' ') in media_len()
215 *dptr != '@' && *dptr != '\r' && *dptr != '\n') { in skp_epaddr_len()
220 if (dptr < limit && *dptr == '@') { in skp_epaddr_len()
257 if (*dptr == '\r' || *dptr == '\n') in ct_sip_parse_request()
325 if (*dptr != ' ' && *dptr != '\t') in sip_follow_continuation()
329 for (; dptr < limit; dptr++) { in sip_follow_continuation()
330 if (*dptr != ' ' && *dptr != '\t') in sip_follow_continuation()
338 for (; dptr < limit; dptr++) { in sip_skip_whitespace()
339 if (*dptr == ' ' || *dptr == '\t') in sip_skip_whitespace()
376 for (dptr += dataoff; dptr < limit; dptr++) { in ct_sip_get_header()
[all …]
A Dnf_nat_sip.c36 const char **dptr, unsigned int *datalen, in mangle_packet() argument
65 *dptr = skb->data + dataoff; in mangle_packet()
94 const char **dptr, unsigned int *datalen, in map_addr() argument
129 const char **dptr, unsigned int *datalen, in map_sip_addr() argument
147 const char **dptr, unsigned int *datalen) in nf_nat_sip() argument
161 if (ct_sip_parse_request(ct, *dptr, *datalen, in nf_nat_sip()
437 const char **dptr, unsigned int *datalen) in mangle_content_len() argument
446 if (ct_sip_get_sdp_header(ct, *dptr, 0, *datalen, in mangle_content_len()
464 const char **dptr, unsigned int *datalen, in mangle_sdp_packet() argument
483 const char **dptr, unsigned int *datalen, in nf_nat_sdp_addr() argument
[all …]
/linux/lib/raid6/
A Davx2.c36 u8 **dptr = (u8 **)ptrs; in raid6_avx21_gen_syndrome() local
41 p = dptr[z0+1]; /* XOR parity */ in raid6_avx21_gen_syndrome()
42 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx21_gen_syndrome()
85 u8 **dptr = (u8 **)ptrs; in raid6_avx21_xor_syndrome() local
90 p = dptr[disks-2]; /* XOR parity */ in raid6_avx21_xor_syndrome()
143 u8 **dptr = (u8 **)ptrs; in raid6_avx22_gen_syndrome() local
148 p = dptr[z0+1]; /* XOR parity */ in raid6_avx22_gen_syndrome()
195 u8 **dptr = (u8 **)ptrs; in raid6_avx22_xor_syndrome() local
228 :: "m" (dptr[z][d+32])); in raid6_avx22_xor_syndrome()
275 u8 **dptr = (u8 **)ptrs; in raid6_avx24_gen_syndrome() local
[all …]
A 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()
90 u8 **dptr = (u8 **)ptrs; in raid6_sse21_xor_syndrome() local
95 p = dptr[disks-2]; /* XOR parity */ in raid6_sse21_xor_syndrome()
148 u8 **dptr = (u8 **)ptrs; in raid6_sse22_gen_syndrome() local
153 p = dptr[z0+1]; /* XOR parity */ in raid6_sse22_gen_syndrome()
154 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse22_gen_syndrome()
201 u8 **dptr = (u8 **)ptrs; in raid6_sse22_xor_syndrome() local
280 u8 **dptr = (u8 **)ptrs; in raid6_sse24_gen_syndrome() local
[all …]
A Davx512.c46 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_gen_syndrome() local
68 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
197 : "m" (dptr[z0][d]), "m" (dptr[z0][d+64])); in raid6_avx5122_gen_syndrome()
218 : "m" (dptr[z][d]), "m" (dptr[z][d+64])); in raid6_avx5122_gen_syndrome()
257 : "m" (dptr[z0][d]), "m" (dptr[z0][d+64]), in raid6_avx5122_xor_syndrome()
280 : "m" (dptr[z][d]), "m" (dptr[z][d+64])); in raid6_avx5122_xor_syndrome()
394 : "m" (dptr[z][d]), "m" (dptr[z][d+64]), in raid6_avx5124_gen_syndrome()
395 "m" (dptr[z][d+128]), "m" (dptr[z][d+192])); in raid6_avx5124_gen_syndrome()
453 : "m" (dptr[z0][d]), "m" (dptr[z0][d+64]), in raid6_avx5124_xor_syndrome()
454 "m" (dptr[z0][d+128]), "m" (dptr[z0][d+192]), in raid6_avx5124_xor_syndrome()
[all …]
A Dloongarch_simd.c35 u8 **dptr = (u8 **)ptrs; in raid6_lsx_gen_syndrome() local
40 p = dptr[z0+1]; /* XOR parity */ in raid6_lsx_gen_syndrome()
41 q = dptr[z0+2]; /* RS syndrome */ in raid6_lsx_gen_syndrome()
117 u8 **dptr = (u8 **)ptrs; in raid6_lsx_xor_syndrome() local
122 p = dptr[disks-2]; /* XOR parity */ in raid6_lsx_xor_syndrome()
123 q = dptr[disks-1]; /* RS syndrome */ in raid6_lsx_xor_syndrome()
266 u8 **dptr = (u8 **)ptrs; in raid6_lasx_gen_syndrome() local
271 p = dptr[z0+1]; /* XOR parity */ in raid6_lasx_gen_syndrome()
272 q = dptr[z0+2]; /* RS syndrome */ in raid6_lasx_gen_syndrome()
326 u8 **dptr = (u8 **)ptrs; in raid6_lasx_xor_syndrome() local
[all …]
A 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()
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
106 p = dptr[z0+1]; /* XOR parity */ in raid6_sse12_gen_syndrome()
107 q = dptr[z0+2]; /* RS syndrome */ in raid6_sse12_gen_syndrome()
[all …]
A 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()
101 asm volatile("movq %0,%%mm3" : : "m" (dptr[z0][d+8])); in raid6_mmx2_gen_syndrome()
113 asm volatile("movq %0,%%mm5" : : "m" (dptr[z][d])); in raid6_mmx2_gen_syndrome()
[all …]
A Ds390vx.uc49 u8 **dptr, *p, *q;
55 dptr = (u8 **) ptrs;
57 p = dptr[z0 + 1]; /* XOR parity */
58 q = dptr[z0 + 2]; /* RS syndrome */
61 LOAD_DATA(0,&dptr[z0][d]);
68 LOAD_DATA(16,&dptr[z][d]);
82 u8 **dptr, *p, *q;
85 dptr = (u8 **) ptrs;
87 p = dptr[disks - 2]; /* XOR parity */
95 LOAD_DATA(0,&dptr[z0][d]);
[all …]
A Dint.uc77 u8 **dptr = (u8 **)ptrs;
84 p = dptr[z0+1]; /* XOR parity */
85 q = dptr[z0+2]; /* RS syndrome */
88 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
90 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
106 u8 **dptr = (u8 **)ptrs;
113 p = dptr[disks-2]; /* XOR parity */
114 q = dptr[disks-1]; /* RS syndrome */
118 wq$$ = wp$$ = *(unative_t *)&dptr[z0][d+$$*NSIZE];
120 wd$$ = *(unative_t *)&dptr[z][d+$$*NSIZE];
A Dneon.uc59 uint8_t **dptr = (uint8_t **)ptrs;
67 p = dptr[z0+1]; /* XOR parity */
68 q = dptr[z0+2]; /* RS syndrome */
71 wq$$ = wp$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
73 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
90 uint8_t **dptr = (uint8_t **)ptrs;
98 p = dptr[disks-2]; /* XOR parity */
99 q = dptr[disks-1]; /* RS syndrome */
102 wq$$ = vld1q_u8(&dptr[z0][d+$$*NSIZE]);
107 wd$$ = vld1q_u8(&dptr[z][d+$$*NSIZE]);
/linux/net/lapb/
A Dlapb_subr.c225 unsigned char *dptr; in lapb_send_control() local
235 *dptr = frametype; in lapb_send_control()
239 dptr[0] = frametype; in lapb_send_control()
245 *dptr = frametype; in lapb_send_control()
261 unsigned char *dptr; in lapb_transmit_frmr() local
270 *dptr++ = LAPB_FRMR; in lapb_transmit_frmr()
276 *dptr |= 0x01; in lapb_transmit_frmr()
277 dptr++; in lapb_transmit_frmr()
285 *dptr++ = LAPB_FRMR; in lapb_transmit_frmr()
290 *dptr |= 0x10; in lapb_transmit_frmr()
[all …]
/linux/net/rose/
A Drose_link.c179 unsigned char *dptr; in rose_transmit_restart_request() local
192 *dptr++ = ROSE_GFI; in rose_transmit_restart_request()
193 *dptr++ = 0x00; in rose_transmit_restart_request()
196 *dptr++ = 0; in rose_transmit_restart_request()
208 unsigned char *dptr; in rose_transmit_restart_confirmation() local
221 *dptr++ = ROSE_GFI; in rose_transmit_restart_confirmation()
222 *dptr++ = 0x00; in rose_transmit_restart_confirmation()
236 unsigned char *dptr; in rose_transmit_clear_request() local
255 *dptr++ = cause; in rose_transmit_clear_request()
256 *dptr++ = diagnostic; in rose_transmit_clear_request()
[all …]
A Drose_subr.c103 unsigned char *dptr; in rose_write_internal() local
141 *dptr++ = lci2; in rose_write_internal()
142 *dptr++ = frametype; in rose_write_internal()
150 dptr += faclen; in rose_write_internal()
155 *dptr++ = lci2; in rose_write_internal()
156 *dptr++ = frametype; in rose_write_internal()
163 *dptr++ = lci2; in rose_write_internal()
171 *dptr++ = lci2; in rose_write_internal()
174 *dptr++ = 0; in rose_write_internal()
180 *dptr++ = lci2; in rose_write_internal()
[all …]
/linux/net/x25/
A Dx25_subr.c113 unsigned char *dptr; in x25_write_internal() local
163 dptr = skb_put(skb, 2); in x25_write_internal()
170 *dptr++ = lci2; in x25_write_internal()
173 *dptr++ = lci2; in x25_write_internal()
182 dptr = skb_put(skb, 1); in x25_write_internal()
220 *dptr++ = frametype; in x25_write_internal()
227 *dptr++ = frametype; in x25_write_internal()
237 *dptr++ = frametype; in x25_write_internal()
241 *dptr = frametype; in x25_write_internal()
249 dptr = skb_put(skb, 1); in x25_write_internal()
[all …]
A Dx25_link.c134 unsigned char *dptr; in x25_transmit_restart_request() local
146 *dptr++ = 0x00; in x25_transmit_restart_request()
148 *dptr++ = 0x00; in x25_transmit_restart_request()
149 *dptr++ = 0; in x25_transmit_restart_request()
161 unsigned char *dptr; in x25_transmit_restart_confirmation() local
173 *dptr++ = 0x00; in x25_transmit_restart_confirmation()
188 unsigned char *dptr; in x25_transmit_clear_request() local
202 *dptr++ = (lci >> 0) & 0xFF; in x25_transmit_clear_request()
203 *dptr++ = X25_CLEAR_REQUEST; in x25_transmit_clear_request()
204 *dptr++ = cause; in x25_transmit_clear_request()
[all …]
/linux/include/linux/netfilter/
A Dnf_conntrack_sip.h45 const char **dptr, unsigned int *datalen,
49 const char **dptr, unsigned int *datalen,
69 const char *dptr, const char *limit,
114 const char **dptr,
123 const char **dptr,
132 const char **dptr,
142 const char **dptr,
151 const char **dptr,
159 const char **dptr,
169 int ct_sip_parse_request(const struct nf_conn *ct, const char *dptr,
[all …]
/linux/net/ax25/
A Dax25_subr.c150 unsigned char *dptr; in ax25_send_control() local
161 dptr = skb_put(skb, 1); in ax25_send_control()
162 *dptr = frametype; in ax25_send_control()
168 dptr = skb_put(skb, 1); in ax25_send_control()
169 *dptr = frametype; in ax25_send_control()
172 dptr = skb_put(skb, 2); in ax25_send_control()
173 dptr[0] = frametype; in ax25_send_control()
190 char *dptr; in ax25_return_dm() local
204 dptr = skb_put(skb, 1); in ax25_return_dm()
206 *dptr = AX25_DM | AX25_PF; in ax25_return_dm()
[all …]
/linux/net/netfilter/ipvs/
A Dip_vs_pe_sip.c30 static int get_callid(const char *dptr, unsigned int dataoff, in get_callid() argument
36 int ret = ct_sip_get_header(NULL, dptr, dataoff, datalen, in get_callid()
56 if (*(dptr + *matchoff + *matchlen) != '\r' && in get_callid()
57 *(dptr + *matchoff + *matchlen) != '\n') in get_callid()
61 IP_VS_DEBUG_CALLID(dptr + *matchoff, *matchlen), in get_callid()
71 const char *dptr; in ip_vs_sip_fill_param() local
89 dptr = skb->data + dataoff; in ip_vs_sip_fill_param()
92 if (get_callid(dptr, 0, datalen, &matchoff, &matchlen)) in ip_vs_sip_fill_param()
98 p->pe_data = kmemdup(dptr + matchoff, matchlen, GFP_ATOMIC); in ip_vs_sip_fill_param()
/linux/lib/
A 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()
/linux/net/ipv4/
A Dip_options.c90 dptr = dopt->__data; in __ip_options_echo()
100 dptr[2] = soffset + 4; in __ip_options_echo()
103 dptr += optlen; in __ip_options_echo()
138 dptr[2] = soffset; in __ip_options_echo()
140 dptr += optlen; in __ip_options_echo()
166 dptr[0] = start[0]; in __ip_options_echo()
167 dptr[1] = doffset+3; in __ip_options_echo()
168 dptr[2] = 4; in __ip_options_echo()
169 dptr += doffset+3; in __ip_options_echo()
179 dptr += optlen; in __ip_options_echo()
[all …]
/linux/tools/testing/selftests/bpf/progs/
A Dverifier_global_subprogs.c361 __weak int subprog_dynptr(struct bpf_dynptr *dptr) in subprog_dynptr() argument
365 d = bpf_dynptr_data(dptr, 0, sizeof(long)); in subprog_dynptr()
371 d = bpf_dynptr_slice(dptr, 0, &buf, sizeof(long)); in subprog_dynptr()
384 struct bpf_dynptr dptr; in arg_tag_dynptr() local
386 bpf_dynptr_from_xdp(ctx, 0, &dptr); in arg_tag_dynptr()
388 return subprog_dynptr(&dptr); in arg_tag_dynptr()
/linux/drivers/gpu/drm/radeon/
A Datom.c602 int dptr = *ptr; in atom_op_add() local
616 int dptr = *ptr; in atom_op_and() local
651 int dptr = *ptr; in atom_op_clear() local
764 int dptr = *ptr; in atom_op_mask() local
781 int dptr = *ptr; in atom_op_move() local
814 int dptr = *ptr; in atom_op_or() local
904 int dptr = *ptr; in atom_op_shift_left() local
920 int dptr = *ptr; in atom_op_shift_right() local
936 int dptr = *ptr; in atom_op_shl() local
955 int dptr = *ptr; in atom_op_shr() local
[all …]

Completed in 52 milliseconds

123