Home
last modified time | relevance | path

Searched refs:datap (Results 1 - 25 of 162) sorted by relevance

1234567

/third_party/elfutils/libdw/
H A Ddwarf_formaddr.c69 const unsigned char *datap; in __libdw_addrx() local
70 datap = dbg->sectiondata[IDX_debug_addr]->d_buf + addr_off + idx; in __libdw_addrx()
72 *addr = read_4ubyte_unaligned (dbg, datap); in __libdw_addrx()
74 *addr = read_8ubyte_unaligned (dbg, datap); in __libdw_addrx()
88 const unsigned char *datap = attr->valp; in dwarf_formaddr() local
94 if (__libdw_read_address (dbg, cu_sec_idx (cu), datap, in dwarf_formaddr()
103 if (datap >= endp) in dwarf_formaddr()
109 get_uleb128 (idx, datap, endp); in dwarf_formaddr()
113 if (datap >= endp - 1) in dwarf_formaddr()
115 idx = *datap; in dwarf_formaddr()
[all...]
H A Ddwarf_formudata.c76 const unsigned char *datap = attr->valp; in __libdw_formptr() local
79 || datap < (const unsigned char *) data->d_buf in __libdw_formptr()
81 || ((size_t) (datap in __libdw_formptr()
87 offset = read_4ubyte_unaligned (attr->cu->dbg, datap); in __libdw_formptr()
89 offset = read_8ubyte_unaligned (attr->cu->dbg, datap); in __libdw_formptr()
144 const unsigned char *datap = attr->valp; in dwarf_formudata() local
150 if (datap + 1 > endp) in dwarf_formudata()
160 if (datap + 2 > endp) in dwarf_formudata()
299 if (datap + 1 > endp) in dwarf_formudata()
301 get_sleb128 (*return_uval, datap, end in dwarf_formudata()
[all...]
H A Ddwarf_formstring.c92 const unsigned char *datap = attrp->valp; in dwarf_formstring() local
98 if (datap >= endp) in dwarf_formstring()
104 get_uleb128 (idx, datap, endp); in dwarf_formstring()
108 if (datap >= endp - 1) in dwarf_formstring()
110 idx = *datap; in dwarf_formstring()
114 if (datap >= endp - 2) in dwarf_formstring()
116 idx = read_2ubyte_unaligned (dbg, datap); in dwarf_formstring()
120 if (datap >= endp - 3) in dwarf_formstring()
122 idx = read_3ubyte_unaligned (dbg, datap); in dwarf_formstring()
126 if (datap > in dwarf_formstring()
[all...]
H A Ddwarf_formsdata.c44 const unsigned char *datap = attr->valp; in dwarf_formsdata() local
50 if (datap + 1 > endp) in dwarf_formsdata()
60 if (datap + 2 > endp) in dwarf_formsdata()
66 if (datap + 4 > endp) in dwarf_formsdata()
72 if (datap + 8 > endp) in dwarf_formsdata()
78 if (datap + 1 > endp) in dwarf_formsdata()
80 get_sleb128 (*return_sval, datap, endp); in dwarf_formsdata()
84 if (datap + 1 > endp) in dwarf_formsdata()
86 get_uleb128 (*return_sval, datap, endp); in dwarf_formsdata()
91 get_sleb128_unchecked (*return_sval, datap); in dwarf_formsdata()
[all...]
H A Ddwarf_formblock.c44 const unsigned char *datap = attr->valp; in dwarf_formblock() local
50 if (unlikely (endp - datap < 1)) in dwarf_formblock()
57 if (unlikely (endp - datap < 2)) in dwarf_formblock()
64 if (unlikely (endp - datap < 4)) in dwarf_formblock()
72 if (unlikely (endp - datap < 1)) in dwarf_formblock()
74 get_uleb128 (return_block->length, datap, endp); in dwarf_formblock()
75 return_block->data = (unsigned char *) datap; in dwarf_formblock()
82 if (unlikely (endp - datap < 16)) in dwarf_formblock()
85 return_block->data = (unsigned char *) datap; in dwarf_formblock()
H A Ddwarf_formref.c41 const unsigned char *datap = attr->valp; in __libdw_formref() local
53 if (datap + 1 > endp) in __libdw_formref()
63 if (datap + 2 > endp) in __libdw_formref()
69 if (datap + 4 > endp) in __libdw_formref()
75 if (datap + 8 > endp) in __libdw_formref()
81 if (datap + 1 > endp) in __libdw_formref()
83 get_uleb128 (*return_offset, datap, endp); in __libdw_formref()
/third_party/FreeBSD/stand/kshim/
H A Dbsd_busspace.c48 uint8_t *datap, bus_size_t count);
50 uint16_t *datap, bus_size_t count);
52 uint32_t *datap, bus_size_t count);
55 uint8_t *datap, bus_size_t count);
57 uint16_t *datap, bus_size_t count);
59 uint32_t *datap, bus_size_t count);
62 uint8_t *datap, bus_size_t count);
64 uint8_t *datap, bus_size_t count);
66 uint32_t *datap, bus_size_t count);
68 uint32_t *datap, bus_size_
71 bus_space_read_multi_1(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint8_t *datap, bus_size_t count) bus_space_read_multi_1() argument
80 bus_space_read_multi_2(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint16_t *datap, bus_size_t count) bus_space_read_multi_2() argument
89 bus_space_read_multi_4(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint32_t *datap, bus_size_t count) bus_space_read_multi_4() argument
100 bus_space_write_multi_1(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint8_t *datap, bus_size_t count) bus_space_write_multi_1() argument
111 bus_space_write_multi_2(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint16_t *datap, bus_size_t count) bus_space_write_multi_2() argument
122 bus_space_write_multi_4(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint32_t *datap, bus_size_t count) bus_space_write_multi_4() argument
172 bus_space_read_region_1(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint8_t *datap, bus_size_t count) bus_space_read_region_1() argument
184 bus_space_write_region_1(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint8_t *datap, bus_size_t count) bus_space_write_region_1() argument
196 bus_space_read_region_4(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint32_t *datap, bus_size_t count) bus_space_read_region_4() argument
218 bus_space_write_region_4(bus_space_tag_t t, bus_space_handle_t h, bus_size_t offset, uint32_t *datap, bus_size_t count) bus_space_write_region_4() argument
[all...]
H A Dbsd_kernel.h142 uint8_t *datap, bus_size_t count);
144 uint16_t *datap, bus_size_t count);
146 uint32_t *datap, bus_size_t count);
149 uint8_t *datap, bus_size_t count);
151 uint16_t *datap, bus_size_t count);
153 uint32_t *datap, bus_size_t count);
156 uint8_t *datap, bus_size_t count);
158 uint8_t *datap, bus_size_t count);
160 uint32_t *datap, bus_size_t count);
162 uint32_t *datap, bus_size_
[all...]
/kernel/linux/linux-6.6/tools/testing/selftests/riscv/vector/
H A Dv_initval_nolibc.c26 char *datap, *tmp; in main() local
28 datap = malloc(MAX_VSIZE); in main()
29 if (!datap) { in main()
34 tmp = datap; in main()
47 : "=&r" (vl), "=r" (tmp) : "r" (datap) : "memory"); in main()
51 if (datap[0] != 0x00 && datap[0] != 0xff) { in main()
53 dump(datap, vl * 4); in main()
58 if (datap[i] != datap[ in main()
[all...]
/kernel/linux/linux-5.10/drivers/net/wireless/ath/ath6kl/
H A Dwmi.c166 u8 *datap; in ath6kl_wmi_dix_2_dot3() local
188 datap = skb->data; in ath6kl_wmi_dix_2_dot3()
192 memcpy(datap, eth_hdr, sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
194 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
310 u8 *datap; in ath6kl_wmi_implicit_create_pstream() local
315 datap = skb->data; in ath6kl_wmi_implicit_create_pstream()
316 data_hdr = (struct wmi_data_hdr *) datap; in ath6kl_wmi_implicit_create_pstream()
327 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + in ath6kl_wmi_implicit_create_pstream()
394 u8 *datap; in ath6kl_wmi_dot11_hdr_remove() local
400 datap in ath6kl_wmi_dot11_hdr_remove()
458 u8 *datap; ath6kl_wmi_dot3_2_dix() local
478 ath6kl_wmi_tx_complete_event_rx(u8 *datap, int len) ath6kl_wmi_tx_complete_event_rx() argument
503 ath6kl_wmi_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_remain_on_chnl_event_rx() argument
535 ath6kl_wmi_cancel_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_cancel_remain_on_chnl_event_rx() argument
573 ath6kl_wmi_tx_status_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_tx_status_event_rx() argument
599 ath6kl_wmi_rx_probe_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_rx_probe_req_event_rx() argument
627 ath6kl_wmi_p2p_capabilities_event_rx(u8 *datap, int len) ath6kl_wmi_p2p_capabilities_event_rx() argument
642 ath6kl_wmi_rx_action_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_rx_action_event_rx() argument
666 ath6kl_wmi_p2p_info_event_rx(u8 *datap, int len) ath6kl_wmi_p2p_info_event_rx() argument
741 ath6kl_wmi_ready_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ready_event_rx() argument
854 ath6kl_wmi_connect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_connect_event_rx() argument
985 ath6kl_wmi_regdomain_event(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_regdomain_event() argument
1020 ath6kl_wmi_disconnect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_disconnect_event_rx() argument
1045 ath6kl_wmi_peer_node_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_peer_node_event_rx() argument
1064 ath6kl_wmi_tkip_micerr_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_tkip_micerr_event_rx() argument
1086 ath6kl_wmi_bssinfo_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_bssinfo_event_rx() argument
1170 ath6kl_wmi_pstream_timeout_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_pstream_timeout_event_rx() argument
1201 ath6kl_wmi_bitrate_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_bitrate_reply_rx() argument
1224 ath6kl_wmi_test_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_test_rx() argument
1231 ath6kl_wmi_ratemask_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ratemask_reply_rx() argument
1241 ath6kl_wmi_ch_list_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ch_list_reply_rx() argument
1251 ath6kl_wmi_tx_pwr_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_tx_pwr_reply_rx() argument
1264 ath6kl_wmi_keepalive_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_keepalive_reply_rx() argument
1274 ath6kl_wmi_scan_complete_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_scan_complete_rx() argument
1287 ath6kl_wmi_neighbor_report_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_neighbor_report_event_rx() argument
1323 ath6kl_wmi_error_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_error_event_rx() argument
1347 ath6kl_wmi_stats_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_stats_event_rx() argument
1408 ath6kl_wmi_rssi_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_rssi_threshold_event_rx() argument
1504 ath6kl_wmi_cac_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_cac_event_rx() argument
1577 ath6kl_wmi_txe_notify_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_txe_notify_event_rx() argument
1661 ath6kl_wmi_snr_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_snr_threshold_event_rx() argument
1751 ath6kl_wmi_aplist_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_aplist_event_rx() argument
3347 ath6kl_wmi_get_pmkid_list_event_rx(struct wmi *wmi, u8 *datap, u32 len) ath6kl_wmi_get_pmkid_list_event_rx() argument
3366 ath6kl_wmi_addba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_addba_req_event_rx() argument
3377 ath6kl_wmi_delba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_delba_req_event_rx() argument
3487 ath6kl_wmi_pspoll_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_pspoll_event_rx() argument
3502 ath6kl_wmi_dtimexpiry_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_dtimexpiry_event_rx() argument
3832 ath6kl_wmi_hb_challenge_resp_event(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_hb_challenge_resp_event() argument
3850 u8 *datap; ath6kl_wmi_control_rx_xtnd() local
3884 ath6kl_wmi_roam_tbl_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_roam_tbl_event_rx() argument
3890 ath6kl_wmi_proc_events_vif(struct wmi *wmi, u16 if_idx, u16 cmd_id, u8 *datap, u32 len) ath6kl_wmi_proc_events_vif() argument
3980 u8 *datap; ath6kl_wmi_proc_events() local
[all...]
/kernel/linux/linux-6.6/drivers/net/wireless/ath/ath6kl/
H A Dwmi.c166 u8 *datap; in ath6kl_wmi_dix_2_dot3() local
188 datap = skb->data; in ath6kl_wmi_dix_2_dot3()
192 memcpy(datap, eth_hdr, sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
194 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + sizeof(*eth_hdr)); in ath6kl_wmi_dix_2_dot3()
310 u8 *datap; in ath6kl_wmi_implicit_create_pstream() local
315 datap = skb->data; in ath6kl_wmi_implicit_create_pstream()
316 data_hdr = (struct wmi_data_hdr *) datap; in ath6kl_wmi_implicit_create_pstream()
327 llc_hdr = (struct ath6kl_llc_snap_hdr *)(datap + in ath6kl_wmi_implicit_create_pstream()
394 u8 *datap; in ath6kl_wmi_dot11_hdr_remove() local
400 datap in ath6kl_wmi_dot11_hdr_remove()
458 u8 *datap; ath6kl_wmi_dot3_2_dix() local
478 ath6kl_wmi_tx_complete_event_rx(u8 *datap, int len) ath6kl_wmi_tx_complete_event_rx() argument
503 ath6kl_wmi_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_remain_on_chnl_event_rx() argument
535 ath6kl_wmi_cancel_remain_on_chnl_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_cancel_remain_on_chnl_event_rx() argument
573 ath6kl_wmi_tx_status_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_tx_status_event_rx() argument
599 ath6kl_wmi_rx_probe_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_rx_probe_req_event_rx() argument
627 ath6kl_wmi_p2p_capabilities_event_rx(u8 *datap, int len) ath6kl_wmi_p2p_capabilities_event_rx() argument
642 ath6kl_wmi_rx_action_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_rx_action_event_rx() argument
666 ath6kl_wmi_p2p_info_event_rx(u8 *datap, int len) ath6kl_wmi_p2p_info_event_rx() argument
741 ath6kl_wmi_ready_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ready_event_rx() argument
854 ath6kl_wmi_connect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_connect_event_rx() argument
985 ath6kl_wmi_regdomain_event(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_regdomain_event() argument
1020 ath6kl_wmi_disconnect_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_disconnect_event_rx() argument
1045 ath6kl_wmi_peer_node_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_peer_node_event_rx() argument
1064 ath6kl_wmi_tkip_micerr_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_tkip_micerr_event_rx() argument
1086 ath6kl_wmi_bssinfo_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_bssinfo_event_rx() argument
1170 ath6kl_wmi_pstream_timeout_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_pstream_timeout_event_rx() argument
1201 ath6kl_wmi_bitrate_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_bitrate_reply_rx() argument
1224 ath6kl_wmi_test_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_test_rx() argument
1231 ath6kl_wmi_ratemask_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ratemask_reply_rx() argument
1241 ath6kl_wmi_ch_list_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_ch_list_reply_rx() argument
1251 ath6kl_wmi_tx_pwr_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_tx_pwr_reply_rx() argument
1264 ath6kl_wmi_keepalive_reply_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_keepalive_reply_rx() argument
1274 ath6kl_wmi_scan_complete_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_scan_complete_rx() argument
1287 ath6kl_wmi_neighbor_report_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_neighbor_report_event_rx() argument
1323 ath6kl_wmi_error_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_error_event_rx() argument
1347 ath6kl_wmi_stats_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_stats_event_rx() argument
1408 ath6kl_wmi_rssi_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_rssi_threshold_event_rx() argument
1504 ath6kl_wmi_cac_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_cac_event_rx() argument
1577 ath6kl_wmi_txe_notify_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_txe_notify_event_rx() argument
1661 ath6kl_wmi_snr_threshold_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_snr_threshold_event_rx() argument
1751 ath6kl_wmi_aplist_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_aplist_event_rx() argument
3333 ath6kl_wmi_get_pmkid_list_event_rx(struct wmi *wmi, u8 *datap, u32 len) ath6kl_wmi_get_pmkid_list_event_rx() argument
3352 ath6kl_wmi_addba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_addba_req_event_rx() argument
3363 ath6kl_wmi_delba_req_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_delba_req_event_rx() argument
3473 ath6kl_wmi_pspoll_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_pspoll_event_rx() argument
3488 ath6kl_wmi_dtimexpiry_event_rx(struct wmi *wmi, u8 *datap, int len, struct ath6kl_vif *vif) ath6kl_wmi_dtimexpiry_event_rx() argument
3818 ath6kl_wmi_hb_challenge_resp_event(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_hb_challenge_resp_event() argument
3836 u8 *datap; ath6kl_wmi_control_rx_xtnd() local
3870 ath6kl_wmi_roam_tbl_event_rx(struct wmi *wmi, u8 *datap, int len) ath6kl_wmi_roam_tbl_event_rx() argument
3876 ath6kl_wmi_proc_events_vif(struct wmi *wmi, u16 if_idx, u16 cmd_id, u8 *datap, u32 len) ath6kl_wmi_proc_events_vif() argument
3966 u8 *datap; ath6kl_wmi_proc_events() local
[all...]
/kernel/linux/linux-6.6/arch/riscv/kvm/
H A Dvcpu_vector.c27 WARN_ON(!cntx->vector.datap); in kvm_riscv_vcpu_vector_reset()
28 memset(cntx->vector.datap, 0, riscv_v_vsize); in kvm_riscv_vcpu_vector_reset()
76 cntx->vector.datap = kmalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context()
77 if (!cntx->vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
80 vcpu->arch.host_context.vector.datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in kvm_riscv_vcpu_alloc_vector_context()
81 if (!vcpu->arch.host_context.vector.datap) in kvm_riscv_vcpu_alloc_vector_context()
89 kfree(vcpu->arch.guest_reset_context.vector.datap); in kvm_riscv_vcpu_free_vector_context()
90 kfree(vcpu->arch.host_context.vector.datap); in kvm_riscv_vcpu_free_vector_context()
118 case KVM_REG_RISCV_VECTOR_CSR_REG(datap): in kvm_riscv_vcpu_vreg_addr()
125 *reg_addr = cntx->vector.datap in kvm_riscv_vcpu_vreg_addr()
[all...]
/third_party/libwebsockets/win32port/dirent/
H A Ddirent-win32.h481 WIN32_FIND_DATAW *datap; in _wreaddir_r() local
484 datap = dirent_next (dirp); in _wreaddir_r()
485 if (datap) { in _wreaddir_r()
495 while (n < PATH_MAX && datap->cFileName[n] != 0) { in _wreaddir_r()
496 entry->d_name[n] = datap->cFileName[n]; in _wreaddir_r()
505 attr = datap->dwFileAttributes; in _wreaddir_r()
590 WIN32_FIND_DATAW *datap; in dirent_first() local
600 datap = &dirp->data; in dirent_first()
607 datap = NULL; in dirent_first()
629 return datap; in dirent_first()
760 WIN32_FIND_DATAW *datap; readdir_r() local
[all...]
/kernel/linux/linux-5.10/arch/m68k/kernel/
H A Dptrace.c167 unsigned long __user *datap = (unsigned long __user *) data; in arch_ptrace() local
195 ret = put_user(tmp, datap); in arch_ptrace()
227 ret = put_user(tmp, datap); in arch_ptrace()
230 datap++; in arch_ptrace()
236 ret = get_user(tmp, datap); in arch_ptrace()
244 datap++; in arch_ptrace()
249 if (copy_to_user(datap, &child->thread.fp, in arch_ptrace()
255 if (copy_from_user(&child->thread.fp, datap, in arch_ptrace()
261 ret = put_user(task_thread_info(child)->tp_value, datap); in arch_ptrace()
/kernel/linux/linux-5.10/drivers/base/
H A Dplatform-msi.c199 struct platform_msi_priv_data *datap; in platform_msi_alloc_priv_data() local
218 datap = kzalloc(sizeof(*datap), GFP_KERNEL); in platform_msi_alloc_priv_data()
219 if (!datap) in platform_msi_alloc_priv_data()
222 datap->devid = ida_simple_get(&platform_msi_devid_ida, in platform_msi_alloc_priv_data()
224 if (datap->devid < 0) { in platform_msi_alloc_priv_data()
225 int err = datap->devid; in platform_msi_alloc_priv_data()
226 kfree(datap); in platform_msi_alloc_priv_data()
230 datap->write_msg = write_msi_msg; in platform_msi_alloc_priv_data()
231 datap in platform_msi_alloc_priv_data()
[all...]
/kernel/linux/linux-6.6/drivers/base/
H A Dplatform-msi.c146 struct platform_msi_priv_data *datap; in platform_msi_alloc_priv_data() local
171 datap = kzalloc(sizeof(*datap), GFP_KERNEL); in platform_msi_alloc_priv_data()
172 if (!datap) in platform_msi_alloc_priv_data()
175 datap->devid = ida_simple_get(&platform_msi_devid_ida, in platform_msi_alloc_priv_data()
177 if (datap->devid < 0) { in platform_msi_alloc_priv_data()
178 err = datap->devid; in platform_msi_alloc_priv_data()
179 kfree(datap); in platform_msi_alloc_priv_data()
183 datap->write_msg = write_msi_msg; in platform_msi_alloc_priv_data()
184 datap in platform_msi_alloc_priv_data()
[all...]
/kernel/linux/linux-6.6/arch/riscv/kernel/
H A Dvector.c85 void *datap; in riscv_v_thread_zalloc() local
87 datap = kzalloc(riscv_v_vsize, GFP_KERNEL); in riscv_v_thread_zalloc()
88 if (!datap) in riscv_v_thread_zalloc()
91 current->thread.vstate.datap = datap; in riscv_v_thread_zalloc()
93 datap)); in riscv_v_thread_zalloc()
157 /* Sanity check. datap should be null by the time of the first-use trap */ in riscv_v_first_use_handler()
158 WARN_ON(current->thread.vstate.datap); in riscv_v_first_use_handler()
H A Dsignal.c77 void __user *datap; in save_v_state() local
83 /* Point datap right after the end of __sc_riscv_v_state */ in save_v_state()
84 datap = state + 1; in save_v_state()
86 /* datap is designed to be 16 byte aligned for better performance */ in save_v_state()
87 WARN_ON(unlikely(!IS_ALIGNED((unsigned long)datap, 16))); in save_v_state()
90 /* Copy everything of vstate but datap. */ in save_v_state()
92 offsetof(struct __riscv_v_ext_state, datap)); in save_v_state()
93 /* Copy the pointer datap itself. */ in save_v_state()
94 err |= __put_user(datap, &state->v_state.datap); in save_v_state()
117 void __user *datap; __restore_v_state() local
[all...]
/kernel/linux/linux-5.10/arch/arm64/kvm/
H A Dmmio.c15 void *datap = NULL; in kvm_mmio_write_buf() local
26 datap = &tmp.byte; in kvm_mmio_write_buf()
30 datap = &tmp.hword; in kvm_mmio_write_buf()
34 datap = &tmp.word; in kvm_mmio_write_buf()
38 datap = &tmp.dword; in kvm_mmio_write_buf()
42 memcpy(buf, datap, len); in kvm_mmio_write_buf()
/kernel/linux/linux-6.6/arch/arm64/kvm/
H A Dmmio.c15 void *datap = NULL; in kvm_mmio_write_buf() local
26 datap = &tmp.byte; in kvm_mmio_write_buf()
30 datap = &tmp.hword; in kvm_mmio_write_buf()
34 datap = &tmp.word; in kvm_mmio_write_buf()
38 datap = &tmp.dword; in kvm_mmio_write_buf()
42 memcpy(buf, datap, len); in kvm_mmio_write_buf()
/kernel/linux/linux-6.6/arch/riscv/include/asm/
H A Dvector.h92 void *datap) in __riscv_v_vstate_save()
110 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_save()
115 void *datap) in __riscv_v_vstate_restore()
132 : "=&r" (vl) : "r" (datap) : "memory"); in __riscv_v_vstate_restore()
171 __riscv_v_vstate_save(vstate, vstate->datap); in riscv_v_vstate_save()
182 __riscv_v_vstate_restore(vstate, vstate->datap); in riscv_v_vstate_restore()
91 __riscv_v_vstate_save(struct __riscv_v_ext_state *save_to, void *datap) __riscv_v_vstate_save() argument
114 __riscv_v_vstate_restore(struct __riscv_v_ext_state *restore_from, void *datap) __riscv_v_vstate_restore() argument
/kernel/linux/linux-6.6/arch/m68k/kernel/
H A Dptrace.c168 unsigned long __user *datap = (unsigned long __user *) data; in arch_ptrace() local
196 ret = put_user(tmp, datap); in arch_ptrace()
228 ret = put_user(tmp, datap); in arch_ptrace()
231 datap++; in arch_ptrace()
237 ret = get_user(tmp, datap); in arch_ptrace()
245 datap++; in arch_ptrace()
250 if (copy_to_user(datap, &child->thread.fp, in arch_ptrace()
256 if (copy_from_user(&child->thread.fp, datap, in arch_ptrace()
262 ret = put_user(task_thread_info(child)->tp_value, datap); in arch_ptrace()
/kernel/linux/linux-5.10/tools/virtio/ringtest/
H A Dptr_ring.c128 int add_inbuf(unsigned len, void *buf, void *datap) in add_inbuf() argument
149 void *datap; in get_buf() local
152 datap = NULL; in get_buf()
154 datap = "Buffer\n"; in get_buf()
158 return datap; in get_buf()
/kernel/linux/linux-6.6/tools/virtio/ringtest/
H A Dptr_ring.c128 int add_inbuf(unsigned len, void *buf, void *datap) in add_inbuf() argument
149 void *datap; in get_buf() local
152 datap = NULL; in get_buf()
154 datap = "Buffer\n"; in get_buf()
158 return datap; in get_buf()
/kernel/linux/linux-5.10/arch/xtensa/kernel/
H A Dptrace.c417 long __user *datap) in ptrace_gethbpregs()
444 if (copy_to_user(datap, user_data, sizeof(user_data))) in ptrace_gethbpregs()
451 long __user *datap) in ptrace_sethbpregs()
464 if (copy_from_user(user_data, datap, sizeof(user_data))) in ptrace_sethbpregs()
503 void __user *datap = (void __user *) data; in arch_ptrace() local
507 ret = ptrace_peekusr(child, addr, datap); in arch_ptrace()
515 ret = ptrace_getregs(child, datap); in arch_ptrace()
519 ret = ptrace_setregs(child, datap); in arch_ptrace()
523 ret = ptrace_getxregs(child, datap); in arch_ptrace()
527 ret = ptrace_setxregs(child, datap); in arch_ptrace()
416 ptrace_gethbpregs(struct task_struct *child, long addr, long __user *datap) ptrace_gethbpregs() argument
450 ptrace_sethbpregs(struct task_struct *child, long addr, long __user *datap) ptrace_sethbpregs() argument
[all...]

Completed in 16 milliseconds

1234567