/Linux-v4.19/net/netrom/ |
D | nr_subr.c | 126 unsigned char *dptr; in nr_write_internal() local 155 dptr = skb_put(skb, skb_tailroom(skb)); in nr_write_internal() 160 *dptr++ = nr->my_index; in nr_write_internal() 161 *dptr++ = nr->my_id; in nr_write_internal() 162 *dptr++ = 0; in nr_write_internal() 163 *dptr++ = 0; in nr_write_internal() 164 *dptr++ = frametype; in nr_write_internal() 165 *dptr++ = nr->window; in nr_write_internal() 166 memcpy(dptr, &nr->user_addr, AX25_ADDR_LEN); in nr_write_internal() 167 dptr[6] &= ~AX25_CBIT; in nr_write_internal() [all …]
|
D | nr_out.c | 191 unsigned char *dptr; in nr_transmit_buffer() local 196 dptr = skb_push(skb, NR_NETWORK_LEN); in nr_transmit_buffer() 198 memcpy(dptr, &nr->source_addr, AX25_ADDR_LEN); in nr_transmit_buffer() 199 dptr[6] &= ~AX25_CBIT; in nr_transmit_buffer() 200 dptr[6] &= ~AX25_EBIT; in nr_transmit_buffer() 201 dptr[6] |= AX25_SSSID_SPARE; in nr_transmit_buffer() 202 dptr += AX25_ADDR_LEN; in nr_transmit_buffer() 204 memcpy(dptr, &nr->dest_addr, AX25_ADDR_LEN); in nr_transmit_buffer() 205 dptr[6] &= ~AX25_CBIT; in nr_transmit_buffer() 206 dptr[6] |= AX25_EBIT; in nr_transmit_buffer() [all …]
|
/Linux-v4.19/net/netfilter/ |
D | nf_conntrack_sip.c | 60 static int string_len(const struct nf_conn *ct, const char *dptr, in string_len() argument 65 while (dptr < limit && isalpha(*dptr)) { in string_len() 66 dptr++; in string_len() 72 static int digits_len(const struct nf_conn *ct, const char *dptr, in digits_len() argument 76 while (dptr < limit && isdigit(*dptr)) { in digits_len() 77 dptr++; in digits_len() 94 static int word_len(const char *dptr, const char *limit) in word_len() argument 97 while (dptr < limit && iswordc(*dptr)) { in word_len() 98 dptr++; in word_len() 104 static int callid_len(const struct nf_conn *ct, const char *dptr, in callid_len() argument [all …]
|
D | nf_nat_sip.c | 34 const char **dptr, unsigned int *datalen, in mangle_packet() argument 63 *dptr = skb->data + dataoff; in mangle_packet() 92 const char **dptr, unsigned int *datalen, in map_addr() argument 121 return mangle_packet(skb, protoff, dataoff, dptr, datalen, in map_addr() 127 const char **dptr, unsigned int *datalen, in map_sip_addr() argument 136 if (ct_sip_parse_header_uri(ct, *dptr, NULL, *datalen, type, NULL, in map_sip_addr() 139 return map_addr(skb, protoff, dataoff, dptr, datalen, in map_sip_addr() 145 const char **dptr, unsigned int *datalen) in nf_nat_sip() argument 158 if (strncasecmp(*dptr, "SIP/2.0", strlen("SIP/2.0")) != 0) { in nf_nat_sip() 159 if (ct_sip_parse_request(ct, *dptr, *datalen, in nf_nat_sip() [all …]
|
/Linux-v4.19/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 | 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 | neon.uc | 59 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]);
|
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];
|
/Linux-v4.19/net/lapb/ |
D | lapb_subr.c | 230 unsigned char *dptr; in lapb_send_control() local 239 dptr = skb_put(skb, 1); in lapb_send_control() 240 *dptr = frametype; in lapb_send_control() 241 *dptr |= poll_bit ? LAPB_SPF : 0; in lapb_send_control() 243 dptr = skb_put(skb, 2); in lapb_send_control() 244 dptr[0] = frametype; in lapb_send_control() 245 dptr[1] = (lapb->vr << 1); in lapb_send_control() 246 dptr[1] |= poll_bit ? LAPB_EPF : 0; in lapb_send_control() 249 dptr = skb_put(skb, 1); in lapb_send_control() 250 *dptr = frametype; in lapb_send_control() [all …]
|
/Linux-v4.19/net/rose/ |
D | rose_link.c | 182 unsigned char *dptr; in rose_transmit_restart_request() local 192 dptr = skb_put(skb, ROSE_MIN_LEN + 3); in rose_transmit_restart_request() 194 *dptr++ = AX25_P_ROSE; in rose_transmit_restart_request() 195 *dptr++ = ROSE_GFI; in rose_transmit_restart_request() 196 *dptr++ = 0x00; in rose_transmit_restart_request() 197 *dptr++ = ROSE_RESTART_REQUEST; in rose_transmit_restart_request() 198 *dptr++ = ROSE_DTE_ORIGINATED; in rose_transmit_restart_request() 199 *dptr++ = 0; in rose_transmit_restart_request() 211 unsigned char *dptr; in rose_transmit_restart_confirmation() local 221 dptr = skb_put(skb, ROSE_MIN_LEN + 1); in rose_transmit_restart_confirmation() [all …]
|
D | rose_subr.c | 106 unsigned char *dptr; in rose_write_internal() local 134 dptr = skb_put(skb, skb_tailroom(skb)); in rose_write_internal() 141 *dptr++ = ROSE_GFI | lci1; in rose_write_internal() 142 *dptr++ = lci2; in rose_write_internal() 143 *dptr++ = frametype; in rose_write_internal() 144 *dptr++ = ROSE_CALL_REQ_ADDR_LEN_VAL; in rose_write_internal() 145 memcpy(dptr, &rose->dest_addr, ROSE_ADDR_LEN); in rose_write_internal() 146 dptr += ROSE_ADDR_LEN; in rose_write_internal() 147 memcpy(dptr, &rose->source_addr, ROSE_ADDR_LEN); in rose_write_internal() 148 dptr += ROSE_ADDR_LEN; in rose_write_internal() [all …]
|
/Linux-v4.19/net/x25/ |
D | x25_subr.c | 118 unsigned char *dptr; in x25_write_internal() local 168 dptr = skb_put(skb, 2); in x25_write_internal() 174 *dptr++ = lci1 | X25_GFI_EXTSEQ; in x25_write_internal() 175 *dptr++ = lci2; in x25_write_internal() 177 *dptr++ = lci1 | X25_GFI_STDSEQ; in x25_write_internal() 178 *dptr++ = lci2; in x25_write_internal() 187 dptr = skb_put(skb, 1); in x25_write_internal() 188 *dptr++ = X25_CALL_REQUEST; in x25_write_internal() 203 dptr = skb_put(skb, 2); in x25_write_internal() 204 *dptr++ = X25_CALL_ACCEPTED; in x25_write_internal() [all …]
|
D | x25_link.c | 119 unsigned char *dptr; in x25_transmit_restart_request() local 128 dptr = skb_put(skb, X25_STD_MIN_LEN + 2); in x25_transmit_restart_request() 130 *dptr++ = nb->extended ? X25_GFI_EXTSEQ : X25_GFI_STDSEQ; in x25_transmit_restart_request() 131 *dptr++ = 0x00; in x25_transmit_restart_request() 132 *dptr++ = X25_RESTART_REQUEST; in x25_transmit_restart_request() 133 *dptr++ = 0x00; in x25_transmit_restart_request() 134 *dptr++ = 0; in x25_transmit_restart_request() 146 unsigned char *dptr; in x25_transmit_restart_confirmation() local 155 dptr = skb_put(skb, X25_STD_MIN_LEN); in x25_transmit_restart_confirmation() 157 *dptr++ = nb->extended ? X25_GFI_EXTSEQ : X25_GFI_STDSEQ; in x25_transmit_restart_confirmation() [all …]
|
/Linux-v4.19/net/ax25/ |
D | ax25_subr.c | 153 unsigned char *dptr; in ax25_send_control() local 164 dptr = skb_put(skb, 1); in ax25_send_control() 165 *dptr = frametype; in ax25_send_control() 166 *dptr |= (poll_bit) ? AX25_PF : 0; in ax25_send_control() 168 *dptr |= (ax25->vr << 5); in ax25_send_control() 171 dptr = skb_put(skb, 1); in ax25_send_control() 172 *dptr = frametype; in ax25_send_control() 173 *dptr |= (poll_bit) ? AX25_PF : 0; in ax25_send_control() 175 dptr = skb_put(skb, 2); in ax25_send_control() 176 dptr[0] = frametype; in ax25_send_control() [all …]
|
/Linux-v4.19/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-v4.19/net/netfilter/ipvs/ |
D | ip_vs_pe_sip.c | 29 static int get_callid(const char *dptr, unsigned int dataoff, in get_callid() argument 35 int ret = ct_sip_get_header(NULL, dptr, dataoff, datalen, in get_callid() 55 if (*(dptr + *matchoff + *matchlen) != '\r' && in get_callid() 56 *(dptr + *matchoff + *matchlen) != '\n') in get_callid() 60 IP_VS_DEBUG_CALLID(dptr + *matchoff, *matchlen), in get_callid() 70 const char *dptr; in ip_vs_sip_fill_param() local 88 dptr = skb->data + dataoff; in ip_vs_sip_fill_param() 91 if (get_callid(dptr, 0, datalen, &matchoff, &matchlen)) in ip_vs_sip_fill_param() 97 p->pe_data = kmemdup(dptr + matchoff, matchlen, GFP_ATOMIC); in ip_vs_sip_fill_param()
|
/Linux-v4.19/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-v4.19/net/ipv4/ |
D | ip_options.c | 93 unsigned char *sptr, *dptr; in __ip_options_echo() local 103 dptr = dopt->__data; in __ip_options_echo() 109 memcpy(dptr, sptr+sopt->rr, optlen); in __ip_options_echo() 113 dptr[2] = soffset + 4; in __ip_options_echo() 116 dptr += optlen; in __ip_options_echo() 123 memcpy(dptr, sptr+sopt->ts, optlen); in __ip_options_echo() 134 if ((dptr[3]&0xF) != IPOPT_TS_PRESPEC) { in __ip_options_echo() 143 memcpy(&addr, dptr+soffset-1, 4); in __ip_options_echo() 151 dptr[2] = soffset; in __ip_options_echo() 153 dptr += optlen; in __ip_options_echo() [all …]
|
/Linux-v4.19/drivers/gpu/drm/radeon/ |
D | atom.c | 586 int dptr = *ptr; in atom_op_add() local 593 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_add() 600 int dptr = *ptr; in atom_op_and() local 607 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_and() 635 int dptr = *ptr; in atom_op_clear() local 640 atom_put_dst(ctx, arg, attr, &dptr, 0, saved); in atom_op_clear() 748 int dptr = *ptr; in atom_op_mask() local 758 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_mask() 765 int dptr = *ptr; in atom_op_move() local 775 atom_put_dst(ctx, arg, attr, &dptr, src, saved); in atom_op_move() [all …]
|
/Linux-v4.19/drivers/gpu/drm/amd/amdgpu/ |
D | atom.c | 582 int dptr = *ptr; in atom_op_add() local 589 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_add() 596 int dptr = *ptr; in atom_op_and() local 603 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_and() 631 int dptr = *ptr; in atom_op_clear() local 636 atom_put_dst(ctx, arg, attr, &dptr, 0, saved); in atom_op_clear() 765 int dptr = *ptr; in atom_op_mask() local 775 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_mask() 782 int dptr = *ptr; in atom_op_move() local 792 atom_put_dst(ctx, arg, attr, &dptr, src, saved); in atom_op_move() [all …]
|