Home
last modified time | relevance | path

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

/linux-4.4.14/net/netrom/
Dnr_subr.c126 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 …]
Dnr_out.c191 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 …]
Dnr_route.c780 unsigned char *dptr; in nr_route_frame() local
846 dptr = skb_push(skb, 1); in nr_route_frame()
847 *dptr = AX25_P_NETROM; in nr_route_frame()
/linux-4.4.14/net/netfilter/
Dnf_conntrack_sip.c58 static int string_len(const struct nf_conn *ct, const char *dptr, in string_len() argument
63 while (dptr < limit && isalpha(*dptr)) { in string_len()
64 dptr++; in string_len()
70 static int digits_len(const struct nf_conn *ct, const char *dptr, in digits_len() argument
74 while (dptr < limit && isdigit(*dptr)) { in digits_len()
75 dptr++; in digits_len()
91 static int word_len(const char *dptr, const char *limit) in word_len() argument
94 while (dptr < limit && iswordc(*dptr)) { in word_len()
95 dptr++; in word_len()
101 static int callid_len(const struct nf_conn *ct, const char *dptr, in callid_len() argument
[all …]
Dnf_nat_sip.c34 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-4.4.14/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 …]
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 …]
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];
/linux-4.4.14/firmware/keyspan_pda/
Dxircom_pgs.S233 mov dptr, #tx_ring
235 movx @dptr, a
236 inc dptr
240 mov dptr, #rx_ring
242 movx @dptr, a
243 inc dptr
248 mov dptr, PORTBCFG
250 movx @dptr, a
251 mov dptr, PORTCCFG
253 movx @dptr, a
[all …]
Dkeyspan_pda.S231 mov dptr, #tx_ring
233 movx @dptr, a
234 inc dptr
238 mov dptr, #rx_ring
240 movx @dptr, a
241 inc dptr
247 mov dptr,OEB
248 movx @dptr,a
251 mov dptr,OUTB
252 movx @dptr,a
[all …]
/linux-4.4.14/net/x25/
Dx25_subr.c118 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()
191 dptr = skb_put(skb, len); in x25_write_internal()
192 memcpy(dptr, addresses, len); in x25_write_internal()
[all …]
Dx25_link.c119 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 …]
Dx25_dev.c208 unsigned char *dptr; in x25_send_frame() local
214 dptr = skb_push(skb, 1); in x25_send_frame()
215 *dptr = X25_IFACE_DATA; in x25_send_frame()
/linux-4.4.14/net/rose/
Drose_link.c184 unsigned char *dptr; in rose_transmit_restart_request() local
194 dptr = skb_put(skb, ROSE_MIN_LEN + 3); in rose_transmit_restart_request()
196 *dptr++ = AX25_P_ROSE; in rose_transmit_restart_request()
197 *dptr++ = ROSE_GFI; in rose_transmit_restart_request()
198 *dptr++ = 0x00; in rose_transmit_restart_request()
199 *dptr++ = ROSE_RESTART_REQUEST; in rose_transmit_restart_request()
200 *dptr++ = ROSE_DTE_ORIGINATED; in rose_transmit_restart_request()
201 *dptr++ = 0; in rose_transmit_restart_request()
213 unsigned char *dptr; in rose_transmit_restart_confirmation() local
223 dptr = skb_put(skb, ROSE_MIN_LEN + 1); in rose_transmit_restart_confirmation()
[all …]
Drose_subr.c106 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-4.4.14/net/lapb/
Dlapb_subr.c232 unsigned char *dptr; in lapb_send_control() local
241 dptr = skb_put(skb, 1); in lapb_send_control()
242 *dptr = frametype; in lapb_send_control()
243 *dptr |= poll_bit ? LAPB_SPF : 0; in lapb_send_control()
245 dptr = skb_put(skb, 2); in lapb_send_control()
246 dptr[0] = frametype; in lapb_send_control()
247 dptr[1] = (lapb->vr << 1); in lapb_send_control()
248 dptr[1] |= poll_bit ? LAPB_EPF : 0; in lapb_send_control()
251 dptr = skb_put(skb, 1); in lapb_send_control()
252 *dptr = frametype; in lapb_send_control()
[all …]
/linux-4.4.14/include/linux/netfilter/
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-4.4.14/net/ax25/
Dax25_subr.c153 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-4.4.14/net/netfilter/ipvs/
Dip_vs_pe_sip.c29 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-4.4.14/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()
136 cd.data = (void *)dptr; in find_cpio_data()
/linux-4.4.14/net/ipv4/
Dip_options.c93 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 …]
Dip_output.c1525 static int ip_reply_glue_bits(void *dptr, char *to, int offset, in ip_reply_glue_bits() argument
1530 csum = csum_partial_copy_nocheck(dptr+offset, to, len, 0); in ip_reply_glue_bits()
/linux-4.4.14/drivers/gpu/drm/radeon/
Datom.c591 int dptr = *ptr; in atom_op_add() local
598 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_add()
605 int dptr = *ptr; in atom_op_and() local
612 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_and()
640 int dptr = *ptr; in atom_op_clear() local
645 atom_put_dst(ctx, arg, attr, &dptr, 0, saved); in atom_op_clear()
753 int dptr = *ptr; in atom_op_mask() local
763 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_mask()
770 int dptr = *ptr; in atom_op_move() local
780 atom_put_dst(ctx, arg, attr, &dptr, src, saved); in atom_op_move()
[all …]
/linux-4.4.14/drivers/gpu/drm/amd/amdgpu/
Datom.c588 int dptr = *ptr; in atom_op_add() local
595 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_add()
602 int dptr = *ptr; in atom_op_and() local
609 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_and()
637 int dptr = *ptr; in atom_op_clear() local
642 atom_put_dst(ctx, arg, attr, &dptr, 0, saved); in atom_op_clear()
771 int dptr = *ptr; in atom_op_mask() local
781 atom_put_dst(ctx, arg, attr, &dptr, dst, saved); in atom_op_mask()
788 int dptr = *ptr; in atom_op_move() local
798 atom_put_dst(ctx, arg, attr, &dptr, src, saved); in atom_op_move()
[all …]
/linux-4.4.14/arch/x86/include/asm/
Dintel_pmc_ipc.h30 u32 *out, u32 outlen, u32 dptr, u32 sptr);
42 u32 *out, u32 outlen, u32 dptr, u32 sptr) in intel_pmc_ipc_raw_cmd() argument
/linux-4.4.14/drivers/net/ethernet/cavium/liquidio/
Docteon_iq.h159 u64 dptr; member
181 u64 dptr; member
Dlio_main.c186 u64 dptr; member
1365 dma_unmap_single(&lio->oct_dev->pci_dev->dev, finfo->dptr, skb->len, in free_netbuf()
1406 finfo->dptr, g->sg_size, in free_netsgbuf()
1454 finfo->dptr, g->sg_size, in free_netsgbuf_with_resp()
2800 ndata.cmd.dptr = dma_map_single(&oct->pci_dev->dev, in liquidio_xmit()
2804 if (dma_mapping_error(&oct->pci_dev->dev, ndata.cmd.dptr)) { in liquidio_xmit()
2810 finfo->dptr = ndata.cmd.dptr; in liquidio_xmit()
2862 ndata.cmd.dptr = dma_map_single(&oct->pci_dev->dev, in liquidio_xmit()
2865 if (dma_mapping_error(&oct->pci_dev->dev, ndata.cmd.dptr)) { in liquidio_xmit()
2874 finfo->dptr = ndata.cmd.dptr; in liquidio_xmit()
[all …]
Drequest_manager.c617 sc->cmd.dptr = sc->dmadptr; in octeon_send_soft_command()
/linux-4.4.14/drivers/net/ethernet/renesas/
Dravb.h658 __le32 dptr; /* Descriptor pointer */ member
686 __le32 dptr; /* Descpriptor pointer */ member
693 __le32 dptr; /* Descpriptor pointer */ member
723 __le32 dptr; /* Descpriptor pointer */ member
Dravb_main.c251 rx_desc->dptr = cpu_to_le32(dma_addr); in ravb_ring_format()
255 rx_desc->dptr = cpu_to_le32((u32)priv->rx_desc_dma[q]); in ravb_ring_format()
266 tx_desc->dptr = cpu_to_le32((u32)priv->tx_desc_dma[q]); in ravb_ring_format()
272 desc->dptr = cpu_to_le32((u32)priv->rx_desc_dma[q]); in ravb_ring_format()
277 desc->dptr = cpu_to_le32((u32)priv->tx_desc_dma[q]); in ravb_ring_format()
444 dma_unmap_single(ndev->dev.parent, le32_to_cpu(desc->dptr), in ravb_tx_free()
547 dma_unmap_single(ndev->dev.parent, le32_to_cpu(desc->dptr), in ravb_rx()
596 desc->dptr = cpu_to_le32(dma_addr); in ravb_rx()
1340 desc->dptr = cpu_to_le32(dma_addr); in ravb_start_xmit()
1350 desc->dptr = cpu_to_le32(dma_addr); in ravb_start_xmit()
[all …]
/linux-4.4.14/drivers/crypto/
Dhifn_795x.c931 u32 dptr = dev->desc_dma; in hifn_init_dma() local
935 dma->cmdr[i].p = __cpu_to_le32(dptr + in hifn_init_dma()
938 dma->resr[i].p = __cpu_to_le32(dptr + in hifn_init_dma()
944 dma->cmdr[HIFN_D_CMD_RSIZE].p = __cpu_to_le32(dptr + in hifn_init_dma()
946 dma->srcr[HIFN_D_SRC_RSIZE].p = __cpu_to_le32(dptr + in hifn_init_dma()
948 dma->dstr[HIFN_D_DST_RSIZE].p = __cpu_to_le32(dptr + in hifn_init_dma()
950 dma->resr[HIFN_D_RES_RSIZE].p = __cpu_to_le32(dptr + in hifn_init_dma()
1026 u32 dptr = dev->desc_dma; in hifn_init_registers() local
1034 hifn_write_1(dev, HIFN_1_DMA_CRAR, dptr + in hifn_init_registers()
1036 hifn_write_1(dev, HIFN_1_DMA_SRAR, dptr + in hifn_init_registers()
[all …]
/linux-4.4.14/drivers/net/wan/
Dz85230.h272 u8 *dptr; /* Pointer into rx buffer */ member
Dz85230.c352 *c->dptr++=ch; in z8530_rx()
366 c->dptr=c->skb->data; in z8530_rx()
1672 c->dptr = c->skb->data; in z8530_rx_done()
/linux-4.4.14/fs/udf/
Dballoc.c469 unsigned char *sptr, *dptr; in udf_table_free_blocks() local
494 dptr = epos.bh->b_data + in udf_table_free_blocks()
496 memcpy(dptr, sptr, adsize); in udf_table_free_blocks()
Dinode.c1894 unsigned char *sptr, *dptr; in udf_add_aext() local
1923 dptr = nbh->b_data + sizeof(struct allocExtDesc); in udf_add_aext()
1924 memcpy(dptr, sptr, adsize); in udf_add_aext()
/linux-4.4.14/drivers/platform/x86/
Dintel_pmc_ipc.c256 u32 outlen, u32 dptr, u32 sptr) in intel_pmc_ipc_raw_cmd() argument
271 writel(dptr, ipcdev.ipc_base + IPC_DPTR); in intel_pmc_ipc_raw_cmd()
/linux-4.4.14/drivers/dma/sh/
Drcar-dmac.c1147 unsigned int dptr = 0; in rcar_dmac_chan_get_residue() local
1167 dptr = (rcar_dmac_chan_read(chan, RCAR_DMACHCRB) & in rcar_dmac_chan_get_residue()
1169 WARN_ON(dptr >= desc->nchunks); in rcar_dmac_chan_get_residue()
1176 if (chunk == running || ++dptr == desc->nchunks) in rcar_dmac_chan_get_residue()
/linux-4.4.14/block/
Dblk-mq.c730 struct list_head *dptr; in __blk_mq_run_hw_queue() local
760 dptr = NULL; in __blk_mq_run_hw_queue()
774 bd.list = dptr; in __blk_mq_run_hw_queue()
801 if (!dptr && rq_list.next != rq_list.prev) in __blk_mq_run_hw_queue()
802 dptr = &driver_list; in __blk_mq_run_hw_queue()
/linux-4.4.14/drivers/video/fbdev/aty/
Daty128fb.c825 u16 dptr; in aty128_map_ROM() local
853 dptr = BIOS_IN16(0x18); in aty128_map_ROM()
880 if (BIOS_IN32(dptr) != (('R' << 24) | ('I' << 16) | ('C' << 8) | 'P')) { in aty128_map_ROM()
882 BIOS_IN32(dptr)); in aty128_map_ROM()
885 rom_type = BIOS_IN8(dptr + 0x14); in aty128_map_ROM()
Dradeon_base.c422 u16 dptr; in radeon_map_ROM() local
456 dptr = BIOS_IN16(0x18); in radeon_map_ROM()
482 if (BIOS_IN32(dptr) != (('R' << 24) | ('I' << 16) | ('C' << 8) | 'P')) { in radeon_map_ROM()
484 "incorrect: %08x\n", pci_name(rinfo->pdev), BIOS_IN32(dptr)); in radeon_map_ROM()
487 rom_type = BIOS_IN8(dptr + 0x14); in radeon_map_ROM()
/linux-4.4.14/sound/aoa/fabrics/
Dlayout.c846 struct layout_dev_ptr *dptr = data; in layout_notify() local
852 ldev = dptr->ptr; in layout_notify()
/linux-4.4.14/drivers/net/wireless/brcm80211/brcmfmac/
Dsdio.c1545 u8 *dptr, num = 0; in brcmf_sdio_rxglom() local
1564 dptr = bus->glomd->data; in brcmf_sdio_rxglom()
1573 sublen = get_unaligned_le16(dptr); in brcmf_sdio_rxglom()
1575 dptr += sizeof(u16); in brcmf_sdio_rxglom()
1732 dptr = (u8 *) (pfirst->data); in brcmf_sdio_rxglom()
1733 sublen = get_unaligned_le16(dptr); in brcmf_sdio_rxglom()
1734 doff = brcmf_sdio_getdatoffset(&dptr[SDPCM_HWHDR_LEN]); in brcmf_sdio_rxglom()
1737 dptr, pfirst->len, in brcmf_sdio_rxglom()
/linux-4.4.14/fs/xfs/
Dxfs_log.c1812 char *dptr; in xlog_sync() local
1825 dptr = (char *)&iclog->ic_header + count; in xlog_sync()
1827 __uint32_t cycle = be32_to_cpu(*(__be32 *)dptr); in xlog_sync()
1830 *(__be32 *)dptr = cpu_to_be32(cycle); in xlog_sync()
1832 dptr += BBSIZE; in xlog_sync()
/linux-4.4.14/fs/gfs2/
Dops_fstype.c447 static int gfs2_lookup_root(struct super_block *sb, struct dentry **dptr, in gfs2_lookup_root() argument
464 *dptr = dentry; in gfs2_lookup_root()
/linux-4.4.14/drivers/input/touchscreen/
Dcyttsp4_core.c57 static void cyttsp4_pr_buf(struct device *dev, u8 *pr_buf, u8 *dptr, int size, in cyttsp4_pr_buf() argument
71 scnprintf(pr_buf + k, CY_MAX_PRBUF_SIZE, fmt, dptr[i]); in cyttsp4_pr_buf()
77 #define cyttsp4_pr_buf(dev, pr_buf, dptr, size, data_name) do { } while (0) argument
/linux-4.4.14/drivers/scsi/qla2xxx/
Dqla_init.c5074 uint32_t *dptr; in qla24xx_nvram_config() local
5102 dptr = (uint32_t *)nv; in qla24xx_nvram_config()
5103 ha->isp_ops->read_nvram(vha, (uint8_t *)dptr, ha->nvram_base, in qla24xx_nvram_config()
5106 chksum += le32_to_cpu(*dptr++); in qla24xx_nvram_config()
6026 uint32_t *dptr; in qla81xx_nvram_config() local
6050 dptr = (uint32_t *)nv; in qla81xx_nvram_config()
6052 chksum += le32_to_cpu(*dptr++); in qla81xx_nvram_config()
/linux-4.4.14/arch/mips/include/asm/octeon/
Dcvmx-sli-defs.h2721 uint64_t dptr:32; member
2723 uint64_t dptr:32;
Dcvmx-npei-defs.h3620 uint64_t dptr:32; member
3622 uint64_t dptr:32;