Searched refs:data_ptr (Results 1 - 25 of 109) sorted by relevance

12345

/freebsd-current/sys/cam/ctl/
H A Dctl_util.h46 void ctl_scsi_inquiry(union ctl_io *io, uint8_t *data_ptr, int32_t data_len,
49 void ctl_scsi_request_sense(union ctl_io *io, uint8_t *data_ptr,
52 void ctl_scsi_report_luns(union ctl_io *io, uint8_t *data_ptr,
55 void ctl_scsi_read_write_buffer(union ctl_io *io, uint8_t *data_ptr,
60 void ctl_scsi_read_write(union ctl_io *io, uint8_t *data_ptr,
65 void ctl_scsi_write_same(union ctl_io *io, uint8_t *data_ptr,
69 void ctl_scsi_read_capacity(union ctl_io *io, uint8_t *data_ptr,
72 void ctl_scsi_read_capacity_16(union ctl_io *io, uint8_t *data_ptr,
75 void ctl_scsi_mode_sense(union ctl_io *io, uint8_t *data_ptr,
87 void ctl_scsi_persistent_res_in(union ctl_io *io, uint8_t *data_ptr,
[all...]
H A Dctl_util.c123 ctl_scsi_inquiry(union ctl_io *io, uint8_t *data_ptr, int32_t data_len, argument
146 ctsio->ext_data_ptr = data_ptr;
153 ctl_scsi_request_sense(union ctl_io *io, uint8_t *data_ptr, argument
174 ctsio->ext_data_ptr = data_ptr;
182 ctl_scsi_report_luns(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, argument
203 ctsio->ext_data_ptr = data_ptr;
211 ctl_scsi_read_write_buffer(union ctl_io *io, uint8_t *data_ptr, argument
242 ctsio->ext_data_ptr = data_ptr;
250 ctl_scsi_read_write(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, argument
343 ctsio->ext_data_ptr = data_ptr;
351 ctl_scsi_write_same(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, uint8_t byte2, uint64_t lba, uint32_t num_blocks, ctl_tag_type tag_type, uint8_t control) argument
382 ctl_scsi_read_capacity(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, uint32_t addr, int reladr, int pmi, ctl_tag_type tag_type, uint8_t control) argument
411 ctl_scsi_read_capacity_16(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, uint64_t addr, int reladr, int pmi, ctl_tag_type tag_type, uint8_t control) argument
443 ctl_scsi_mode_sense(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, int dbd, int llbaa, uint8_t page_code, uint8_t pc, uint8_t subpage, int minimum_cdb_size, ctl_tag_type tag_type, uint8_t control) argument
571 ctl_scsi_persistent_res_in(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, int action, ctl_tag_type tag_type, uint8_t control) argument
597 ctl_scsi_persistent_res_out(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, int action, int type, uint64_t key, uint64_t sa_key, ctl_tag_type tag_type, uint8_t control) argument
655 ctl_scsi_maintenance_in(union ctl_io *io, uint8_t *data_ptr, uint32_t data_len, uint8_t action, ctl_tag_type tag_type, uint8_t control) argument
[all...]
/freebsd-current/sys/dev/mmc/
H A Dmmc_ioctl.h41 uint64_t data_ptr; member in struct:mmc_ioc_cmd
45 (mic).data_ptr = (uint64_t)(uintptr_t)(ptr)
/freebsd-current/sys/dev/usb/
H A Dusb_mbuf.c68 uint8_t *data_ptr; local
80 data_ptr = (void *)(m_ptr + nblocks);
84 m_ptr->min_data_ptr = data_ptr;
92 data_ptr += block_size;
H A Dusb_msctest.c166 uint8_t *data_ptr; member in struct:bbb_transfer
357 sc->data_ptr += actlen;
376 usbd_xfer_set_frame_data(xfer, 0, sc->data_ptr, max_bulk);
409 sc->data_ptr += actlen;
428 usbd_xfer_set_frame_data(xfer, 0, sc->data_ptr, max_bulk);
504 sc->data_ptr += actlen;
523 usbd_xfer_set_frame_data(xfer, 0, sc->data_ptr, max_bulk);
542 void *data_ptr, size_t data_len, void *cmd_ptr, size_t cmd_len,
547 sc->data_ptr = data_ptr;
541 bbb_command_start(struct bbb_transfer *sc, uint8_t dir, uint8_t lun, void *data_ptr, size_t data_len, void *cmd_ptr, size_t cmd_len, usb_timeout_t data_timeout) argument
576 bbb_raw_write(struct bbb_transfer *sc, const void *data_ptr, size_t data_len, usb_timeout_t data_timeout) argument
[all...]
/freebsd-current/tools/tools/vhba/faulty/
H A Dvhba_faulty.c274 memcpy(csio->data_ptr, junk, data_len);
293 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
295 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
309 csio->data_ptr[0] = 0xff;
310 csio->data_ptr[1] = 0xff;
311 csio->data_ptr[2] = 0xff;
312 csio->data_ptr[3] = 0xff;
316 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
317 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
318 csio->data_ptr[
[all...]
/freebsd-current/tools/tools/vhba/lots/
H A Dvhba_lots.c260 memcpy(csio->data_ptr, junk, data_len);
279 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
281 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
295 csio->data_ptr[0] = 0xff;
296 csio->data_ptr[1] = 0xff;
297 csio->data_ptr[2] = 0xff;
298 csio->data_ptr[3] = 0xff;
302 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
303 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
304 csio->data_ptr[
[all...]
/freebsd-current/tools/tools/vhba/medium/
H A Dvhba_medium.c260 memcpy(csio->data_ptr, junk, data_len);
279 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
281 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
296 csio->data_ptr[0] = 0xff;
297 csio->data_ptr[1] = 0xff;
298 csio->data_ptr[2] = 0xff;
299 csio->data_ptr[3] = 0xff;
303 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
304 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
305 csio->data_ptr[
[all...]
/freebsd-current/tools/tools/vhba/rptluns/
H A Dvhba_rptluns.c289 memcpy(csio->data_ptr, junk, data_len);
308 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
310 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
325 csio->data_ptr[0] = 0xff;
326 csio->data_ptr[1] = 0xff;
327 csio->data_ptr[2] = 0xff;
328 csio->data_ptr[3] = 0xff;
332 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
333 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
334 csio->data_ptr[
[all...]
/freebsd-current/tools/tools/vhba/simple/
H A Dvhba_simple.c260 memcpy(csio->data_ptr, junk, data_len);
279 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
281 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
296 csio->data_ptr[0] = 0xff;
297 csio->data_ptr[1] = 0xff;
298 csio->data_ptr[2] = 0xff;
299 csio->data_ptr[3] = 0xff;
303 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
304 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
305 csio->data_ptr[
[all...]
/freebsd-current/tools/tools/vhba/mptest/
H A Dvhba_mptest.c300 memcpy(csio->data_ptr, junk, data_len);
324 memcpy(csio->data_ptr, &vhbas->disk[off], data_len);
326 memcpy(&vhbas->disk[off], csio->data_ptr, data_len);
340 csio->data_ptr[0] = 0xff;
341 csio->data_ptr[1] = 0xff;
342 csio->data_ptr[2] = 0xff;
343 csio->data_ptr[3] = 0xff;
347 csio->data_ptr[0] = (last_blk >> 24) & 0xff;
348 csio->data_ptr[1] = (last_blk >> 16) & 0xff;
349 csio->data_ptr[
[all...]
/freebsd-current/sys/cam/
H A Dcam.c581 void *data_ptr; local
591 data_ptr = csio->data_ptr;
600 data_ptr = ctio->data_ptr;
609 data_ptr = ataio->data_ptr;
619 data_ptr = nvmeio->data_ptr;
631 return (memdesc_vaddr(data_ptr, dxfer_le
[all...]
H A Dcam_ccb.h759 uint8_t *data_ptr; /* Ptr to the data buf/SG list */ member in struct:ccb_scsiio
802 uint8_t *data_ptr; /* Ptr to the data buf/SG list */ member in struct:ccb_ataio
863 uint8_t *data_ptr; /* Ptr to the data buf/SG list */ member in struct:ccb_nvmeio
1294 uint8_t *data_ptr; /* Pointer to the data buf/SG list */ member in struct:ccb_eng_exec
1406 uint8_t *data_ptr, uint32_t dxfer_len,
1416 csio->data_ptr = data_ptr;
1431 u_int init_id, u_int scsi_status, uint8_t *data_ptr,
1440 csio->data_ptr = data_ptr;
1403 cam_fill_csio(struct ccb_scsiio *csio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t flags, uint8_t tag_action, uint8_t *data_ptr, uint32_t dxfer_len, uint8_t sense_len, uint8_t cdb_len, uint32_t timeout) argument
1428 cam_fill_ctio(struct ccb_scsiio *csio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t flags, u_int tag_action, u_int tag_id, u_int init_id, u_int scsi_status, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
1450 cam_fill_ataio(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t flags, u_int tag_action __unused, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
1542 cam_fill_nvmeio(struct ccb_nvmeio *nvmeio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t flags, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
1557 cam_fill_nvmeadmin(struct ccb_nvmeio *nvmeio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t flags, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
[all...]
/freebsd-current/usr.bin/mkimg/
H A Dvhdx.c323 int header_ptr, data_ptr; local
338 data_ptr = SIZE_64KB;
342 le32enc(&entry.offset, data_ptr);
347 le32enc(metadata + data_ptr, PAYLOAD_BLOCK_SIZE);
348 data_ptr += 4;
349 le32enc(metadata + data_ptr, 0);
350 data_ptr += 4;
354 le32enc(&entry.offset, data_ptr);
359 le64enc(metadata + data_ptr, image_size);
360 data_ptr
[all...]
/freebsd-current/sys/cam/ata/
H A Data_all.h134 uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout);
163 uint8_t *data_ptr, uint16_t allocation_length, uint32_t timeout);
167 uint8_t tag_action, uint8_t *data_ptr, uint16_t param_list_length,
173 uint8_t *data_ptr, uint16_t allocation_length, uint32_t timeout);
177 uint8_t tag_action, uint8_t *data_ptr, uint16_t param_list_length,
183 uint8_t zone_flags, uint16_t sector_count, uint8_t *data_ptr,
189 uint8_t zone_flags, uint8_t *data_ptr, uint32_t dxfer_len,
H A Data_all.c732 uint32_t protocol, uint8_t *data_ptr, uint32_t dxfer_len,
742 /*data_ptr*/ data_ptr,
1039 uint8_t *data_ptr, uint16_t length, uint32_t timeout)
1049 data_ptr,
1059 uint8_t tag_action, uint8_t *data_ptr, uint16_t length, uint32_t timeout)
1069 data_ptr,
1073 length > 0 ? data_ptr[0] : 0, 0x82, length / 4);
1080 uint8_t *data_ptr, uint16_t length, uint32_t timeout)
1090 data_ptr,
729 ata_read_log(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint32_t log_address, uint32_t page_number, uint16_t block_count, uint32_t protocol, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
1036 semb_receive_diagnostic_results(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb*), uint8_t tag_action, int pcv, uint8_t page_code, uint8_t *data_ptr, uint16_t length, uint32_t timeout) argument
1057 semb_send_diagnostic(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint8_t tag_action, uint8_t *data_ptr, uint16_t length, uint32_t timeout) argument
1077 semb_read_buffer(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb*), uint8_t tag_action, uint8_t page_code, uint8_t *data_ptr, uint16_t length, uint32_t timeout) argument
1098 semb_write_buffer(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), uint8_t tag_action, uint8_t *data_ptr, uint16_t length, uint32_t timeout) argument
1118 ata_zac_mgmt_out(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), int use_ncq, uint8_t zm_action, uint64_t zone_id, uint8_t zone_flags, uint16_t sector_count, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
1198 ata_zac_mgmt_in(struct ccb_ataio *ataio, uint32_t retries, void (*cbfcnp)(struct cam_periph *, union ccb *), int use_ncq, uint8_t zm_action, uint64_t zone_id, uint8_t zone_flags, uint8_t *data_ptr, uint32_t dxfer_len, uint32_t timeout) argument
[all...]
/freebsd-current/contrib/llvm-project/lldb/source/Plugins/Language/ObjC/
H A DNSDictionary.cpp714 uint64_t *data_ptr = (uint64_t *)buffer_sp->GetBytes(); local
715 *data_ptr = dict_item.key_ptr;
716 *(data_ptr + 1) = dict_item.val_ptr;
718 uint32_t *data_ptr = (uint32_t *)buffer_sp->GetBytes(); local
719 *data_ptr = dict_item.key_ptr;
720 *(data_ptr + 1) = dict_item.val_ptr;
844 uint32_t *data_ptr = reinterpret_cast<uint32_t *>(buffer_sp->GetBytes()); local
845 *data_ptr = dict_item.key_ptr;
846 *(data_ptr + 1) = dict_item.val_ptr;
849 uint64_t *data_ptr local
962 uint64_t *data_ptr = (uint64_t *)buffer_sp->GetBytes(); local
966 uint32_t *data_ptr = (uint32_t *)buffer_sp->GetBytes(); local
1039 uint64_t *data_ptr = (uint64_t *)buffer_sp->GetBytes(); local
1043 uint32_t *data_ptr = (uint32_t *)buffer_sp->GetBytes(); local
1203 uint64_t *data_ptr = (uint64_t *)buffer_sp->GetBytes(); local
1207 uint32_t *data_ptr = (uint32_t *)buffer_sp->GetBytes(); local
1356 uint64_t *data_ptr = (uint64_t *)buffer_sp->GetBytes(); local
1360 uint32_t *data_ptr = (uint32_t *)buffer_sp->GetBytes(); local
[all...]
/freebsd-current/contrib/arm-optimized-routines/pl/math/
H A Dv_atan2_3u.c58 const struct data *data_ptr = ptr_barrier (&data); local
84 shift = vmulq_f64 (shift, data_ptr->pi_over_2);
96 = vfmaq_f64 (v_estrin_7_f64 (z2, x2, x4, data_ptr->poly),
97 v_estrin_11_f64 (z2, x2, x4, x8, data_ptr->poly + 8), x8);
H A Dv_atan2f_3u.c51 const struct data *data_ptr = ptr_barrier (&data); local
77 shift = vmulq_f32 (shift, data_ptr->pi_over_2);
90 v_pairwise_poly_3_f32 (z2, z4, data_ptr->poly), z4,
91 vmulq_f32 (z4, v_pairwise_poly_3_f32 (z2, z4, data_ptr->poly + 4)));
H A Dsv_atan2_2u5.c56 const struct data *data_ptr = ptr_barrier (&data); local
83 shift = svmul_x (pg, shift, data_ptr->pi_over_2);
92 pg, sv_estrin_7_f64_x (pg, z2, x2, x4, data_ptr->poly),
93 sv_estrin_11_f64_x (pg, z2, x2, x4, x8, data_ptr->poly + 8), x8);
H A Dsv_atan2f_3u.c51 const struct data *data_ptr = ptr_barrier (&data); local
78 shift = svmul_x (pg, shift, sv_f32 (data_ptr->pi_over_2));
85 svfloat32_t ret = sv_estrin_7_f32_x (pg, z2, z4, z8, data_ptr->poly);
/freebsd-current/sbin/camcontrol/
H A Dzone.c124 zone_print_status zone_rz_print(uint8_t *data_ptr, uint32_t valid_len,
130 zone_rz_print(uint8_t *data_ptr, uint32_t valid_len, int ata_format, argument
148 hdr = (struct scsi_report_zones_hdr *)data_ptr;
327 uint8_t *data_ptr = NULL; local
439 data_ptr = malloc(alloc_len);
440 if (data_ptr == NULL)
444 bzero(data_ptr, alloc_len);
456 /*data_ptr*/ data_ptr,
506 /*data_ptr*/ data_pt
[all...]
/freebsd-current/contrib/opencsd/decoder/include/common/
H A Dtrc_gen_elem.h82 void setExtendedDataPtr(const void *data_ptr);
208 inline void OcsdTraceElement::setExtendedDataPtr(const void *data_ptr) argument
211 ptr_extended_data = data_ptr;
/freebsd-current/lib/libcam/
H A Dscsi_cmdparse.c675 retval = do_buff_decode(csio->data_ptr, (size_t)csio->dxfer_len,
696 return (do_buff_decode(csio->data_ptr, (size_t)csio->dxfer_len,
736 csio_build(struct ccb_scsiio *csio, uint8_t *data_ptr, uint32_t dxfer_len, argument
760 /* data_ptr */ data_ptr,
773 csio_build_visit(struct ccb_scsiio *csio, uint8_t *data_ptr, argument
802 /* data_ptr */ data_ptr,
822 retval = do_encode(csio->data_ptr, csio->dxfer_len, NULL, NULL, NULL,
857 return (do_encode(csio->data_ptr, csi
[all...]
H A Dcamlib.h162 int csio_build(struct ccb_scsiio *csio, uint8_t *data_ptr,
165 int csio_build_visit(struct ccb_scsiio *csio, uint8_t *data_ptr,

Completed in 310 milliseconds

12345