Home
last modified time | relevance | path

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

123

/linux/net/netfilter/
H A Dnf_conntrack_sip.c66 static int string_len(const struct nf_conn *ct, const char *dptr, in string_len() argument
71 while (dptr < limit && isalpha(*dptr)) { in string_len()
72 dptr++; in string_len()
78 static int digits_len(const struct nf_conn *ct, const char *dptr, in digits_len() argument
82 while (dptr < limit && isdigit(*dptr)) { in digits_len()
83 dptr++; in digits_len()
100 static int word_len(const char *dptr, const char *limit) in word_len() argument
103 while (dptr < limit && iswordc(*dptr)) { in word_len()
104 dptr++; in word_len()
110 static int callid_len(const struct nf_conn *ct, const char *dptr, in callid_len() argument
[all …]
H A Dnf_nat_sip.c36 const char **dptr, unsigned int *datalen, in mangle_packet() argument
65 *dptr = skb->data + dataoff; in mangle_packet()
96 const char **dptr, unsigned int *datalen, in map_addr() argument
125 return mangle_packet(skb, protoff, dataoff, dptr, datalen, in map_addr()
131 const char **dptr, unsigned int *datalen, in map_sip_addr() argument
140 if (ct_sip_parse_header_uri(ct, *dptr, NULL, *datalen, type, NULL, in map_sip_addr()
143 return map_addr(skb, protoff, dataoff, dptr, datalen, in map_sip_addr()
149 const char **dptr, unsigned int *datalen) in nf_nat_sip() argument
162 if (strncasecmp(*dptr, "SIP/2.0", strlen("SIP/2.0")) != 0) { in nf_nat_sip()
163 if (ct_sip_parse_request(ct, *dptr, *datalen, in nf_nat_sip()
[all …]
/linux/lib/raid6/
H 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()
50 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
51 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
54 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
63 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
85 u8 **dptr = (u8 **)ptrs; in raid6_avx21_xor_syndrome() local
[all …]
H A Drvv.c20 u8 **dptr = (u8 **)ptrs; in raid6_rvv1_gen_syndrome_real() local
26 p = dptr[z0 + 1]; /* XOR parity */ in raid6_rvv1_gen_syndrome_real()
27 q = dptr[z0 + 2]; /* RS syndrome */ in raid6_rvv1_gen_syndrome_real()
47 [wp0]"r"(&dptr[z0][d + 0 * nsize]) in raid6_rvv1_gen_syndrome_real()
71 [wd0]"r"(&dptr[z][d + 0 * nsize]), in raid6_rvv1_gen_syndrome_real()
95 u8 **dptr = (u8 **)ptrs; in raid6_rvv1_xor_syndrome_real() local
101 p = dptr[disks - 2]; /* XOR parity */ in raid6_rvv1_xor_syndrome_real()
102 q = dptr[disks - 1]; /* RS syndrome */ in raid6_rvv1_xor_syndrome_real()
122 [wp0]"r"(&dptr[z0][d + 0 * nsize]) in raid6_rvv1_xor_syndrome_real()
147 [wd0]"r"(&dptr[z][d + 0 * nsize]), in raid6_rvv1_xor_syndrome_real()
[all …]
H 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()
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 …]
H A Davx512.c44 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_gen_syndrome() local
49 p = dptr[z0+1]; /* XOR parity */ in raid6_avx5121_gen_syndrome()
50 q = dptr[z0+2]; /* RS syndrome */ in raid6_avx5121_gen_syndrome()
66 : "m" (dptr[z0][d]), "m" (dptr[z0-1][d])); in raid6_avx5121_gen_syndrome()
78 : "m" (dptr[z][d])); in raid6_avx5121_gen_syndrome()
102 u8 **dptr = (u8 **)ptrs; in raid6_avx5121_xor_syndrome() local
107 p = dptr[disks-2]; /* XOR parity */ in raid6_avx5121_xor_syndrome()
108 q = dptr[disks-1]; /* RS syndrome */ in raid6_avx5121_xor_syndrome()
120 : "m" (dptr[z0][d]), "m" (p[d])); in raid6_avx5121_xor_syndrome()
133 : "m" (dptr[z][d])); in raid6_avx5121_xor_syndrome()
[all …]
H 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()
54 asm volatile("vld $vr0, %0" : : "m"(dptr[z0][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
55 asm volatile("vld $vr1, %0" : : "m"(dptr[z0][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
56 asm volatile("vld $vr2, %0" : : "m"(dptr[z0][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
57 asm volatile("vld $vr3, %0" : : "m"(dptr[z0][d+3*NSIZE])); in raid6_lsx_gen_syndrome()
64 asm volatile("vld $vr8, %0" : : "m"(dptr[z][d+0*NSIZE])); in raid6_lsx_gen_syndrome()
65 asm volatile("vld $vr9, %0" : : "m"(dptr[z][d+1*NSIZE])); in raid6_lsx_gen_syndrome()
66 asm volatile("vld $vr10, %0" : : "m"(dptr[z][d+2*NSIZE])); in raid6_lsx_gen_syndrome()
[all …]
H 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()
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 …]
H 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()
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 …]
H A Ds390vx.uc50 u8 **dptr, *p, *q;
56 dptr = (u8 **) ptrs;
58 p = dptr[z0 + 1]; /* XOR parity */
59 q = dptr[z0 + 2]; /* RS syndrome */
62 LOAD_DATA(0,&dptr[z0][d]);
69 LOAD_DATA(16,&dptr[z][d]);
83 u8 **dptr, *p, *q;
86 dptr = (u8 **) ptrs;
88 p = dptr[disks - 2]; /* XOR parity */
89 q = dptr[disk
[all...]
H 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];
H 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]);
H A 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];
H A 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];
/linux/net/lapb/
H A Dlapb_subr.c225 unsigned char *dptr; in lapb_send_control() local
234 dptr = skb_put(skb, 1); in lapb_send_control()
235 *dptr = frametype; in lapb_send_control()
236 *dptr |= poll_bit ? LAPB_SPF : 0; in lapb_send_control()
238 dptr = skb_put(skb, 2); in lapb_send_control()
239 dptr[0] = frametype; in lapb_send_control()
240 dptr[1] = (lapb->vr << 1); in lapb_send_control()
241 dptr[1] |= poll_bit ? LAPB_EPF : 0; in lapb_send_control()
244 dptr = skb_put(skb, 1); in lapb_send_control()
245 *dptr = frametype; in lapb_send_control()
[all …]
/linux/net/x25/
H A Dx25_subr.c114 unsigned char *dptr; in x25_write_internal() local
164 dptr = skb_put(skb, 2); in x25_write_internal()
170 *dptr++ = lci1 | X25_GFI_EXTSEQ; in x25_write_internal()
171 *dptr++ = lci2; in x25_write_internal()
173 *dptr++ = lci1 | X25_GFI_STDSEQ; in x25_write_internal()
174 *dptr++ = lci2; in x25_write_internal()
183 dptr = skb_put(skb, 1); in x25_write_internal()
184 *dptr++ = X25_CALL_REQUEST; in x25_write_internal()
199 dptr = skb_put(skb, 2); in x25_write_internal()
200 *dptr++ = X25_CALL_ACCEPTED; in x25_write_internal()
[all …]
H A Dx25_link.c134 unsigned char *dptr; in x25_transmit_restart_request() local
143 dptr = skb_put(skb, X25_STD_MIN_LEN + 2); in x25_transmit_restart_request()
145 *dptr++ = nb->extended ? X25_GFI_EXTSEQ : X25_GFI_STDSEQ; in x25_transmit_restart_request()
146 *dptr++ = 0x00; in x25_transmit_restart_request()
147 *dptr++ = X25_RESTART_REQUEST; 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
170 dptr = skb_put(skb, X25_STD_MIN_LEN); in x25_transmit_restart_confirmation()
172 *dptr++ = nb->extended ? X25_GFI_EXTSEQ : X25_GFI_STDSEQ; in x25_transmit_restart_confirmation()
[all …]
H A Dx25_dev.c175 unsigned char *dptr; in x25_send_frame() local
181 dptr = skb_push(skb, 1); in x25_send_frame()
182 *dptr = X25_IFACE_DATA; in x25_send_frame()
/linux/include/linux/netfilter/
H 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/lib/
H 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/tools/testing/selftests/bpf/progs/
H A Dverifier_global_subprogs.c454 __weak int subprog_dynptr(struct bpf_dynptr *dptr)
458 d = bpf_dynptr_data(dptr, 0, sizeof(long));
464 d = bpf_dynptr_slice(dptr, 0, &buf, sizeof(long));
477 struct bpf_dynptr dptr;
479 bpf_dynptr_from_xdp(ctx, 0, &dptr);
481 return subprog_dynptr(&dptr);
361 subprog_dynptr(struct bpf_dynptr * dptr) subprog_dynptr() argument
384 struct bpf_dynptr dptr; arg_tag_dynptr() local
H A Dverifier_map_in_map.c220 struct bpf_dynptr dptr; member
235 bpf_ringbuf_reserve_dynptr(rb, sz, 0, &rb_ctx.dptr); in __rb_event_reserve()
249 bpf_ringbuf_submit_dynptr(&ctx->dptr, 0); in __rb_event_submit()
/linux/drivers/gpu/drm/radeon/
H A Datom.c602 int dptr = *ptr; in atom_op_add() local
609 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_add()
616 int dptr = *ptr; in atom_op_and() local
623 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_and()
651 int dptr = *ptr; in atom_op_clear() local
656 atom_put_dst(ctx, arg, attr, &dptr, 0, saved); in atom_op_clear()
764 int dptr = *ptr; in atom_op_mask() local
774 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_mask()
781 int dptr = *ptr; in atom_op_move() local
791 atom_put_dst(ctx, arg, attr, &dptr, src, saved); in atom_op_move()
[all …]
/linux/net/ife/
H A Dife.c163 char *dptr = (char *) tlv + NLA_HDRLEN; in ife_tlv_meta_encode() local
167 memset(dptr, 0, totlen - NLA_HDRLEN); in ife_tlv_meta_encode()
168 memcpy(dptr, dval, dlen); in ife_tlv_meta_encode()
/linux/drivers/net/ethernet/cavium/liquidio/
H A Docteon_iq.h187 u64 dptr; member
209 u64 dptr; member
233 u64 dptr; member

123