/qemu/hw/ide/ |
H A D | atapi.c | 77 buf[0] = 0x00; in cd_data_to_raw() 79 buf[11] = 0x00; in cd_data_to_raw() 80 buf += 12; in cd_data_to_raw() 84 buf += 4; in cd_data_to_raw() 86 buf += 2048; in cd_data_to_raw() 155 void *buf; in cd_read_sector() local 597 buf[6] = 0; in event_status_media() 598 buf[7] = 0; in event_status_media() 819 if (buf[2] != 0 || buf[3] != 0) { in cmd_get_configuration() 1013 nb_sectors = (buf[6] << 16) | (buf[7] << 8) | buf[8]; in cmd_read_cd() [all …]
|
/qemu/contrib/vhost-user-gpu/ |
H A D | vugbm.c | 16 buf->mmap = g_malloc(buf->width * buf->height * 4); in mem_alloc_bo() 17 buf->stride = buf->width * 4; in mem_alloc_bo() 24 g_free(buf->mmap); in mem_free_bo() 69 ret = ftruncate(buf->memfd, udmabuf_get_size(buf)); in udmabuf_alloc_bo() 81 buf->stride = buf->width * 4; in udmabuf_alloc_bo() 95 buf->mmap = mmap(NULL, udmabuf_get_size(buf), in udmabuf_map_bo() 121 munmap(buf->mmap, udmabuf_get_size(buf)); in udmabuf_unmap_bo() 139 buf->bo = gbm_bo_create(dev, buf->width, buf->height, in alloc_bo() 144 buf->stride = gbm_bo_get_stride(buf->bo); in alloc_bo() 162 buf->mmap = gbm_bo_map(buf->bo, 0, 0, buf->width, buf->height, in map_bo() [all …]
|
/qemu/accel/tcg/ |
H A D | monitor.c | 24 static void dump_drift_info(GString *buf) in dump_drift_info() argument 43 static void dump_accel_info(GString *buf) in dump_accel_info() argument 144 static void tcg_dump_info(GString *buf) in tcg_dump_info() argument 149 static void dump_exec_info(GString *buf) in dump_exec_info() argument 186 print_qht_statistics(hst, buf); in dump_exec_info() 199 tcg_dump_info(buf); in dump_exec_info() 211 dump_accel_info(buf); in qmp_x_query_jit() 212 dump_exec_info(buf); in qmp_x_query_jit() 213 dump_drift_info(buf); in qmp_x_query_jit() 218 static void tcg_dump_op_count(GString *buf) in tcg_dump_op_count() argument [all …]
|
/qemu/tests/qtest/ |
H A D | npcm7xx_rng-test.c | 137 vn_obs += (test_bit(k, buf) ^ test_bit(k + 1, buf)); in calc_runs_p() 198 g_assert_cmpfloat(calc_monobit_p(buf, sizeof(buf)), >, 0.01); in test_continuous_monobit() 199 dump_buf_if_failed(buf, sizeof(buf)); in test_continuous_monobit() 211 } buf; in test_continuous_runs() local 220 g_assert_cmpfloat(calc_runs_p(buf.l, sizeof(buf) * BITS_PER_BYTE), >, 0.01); in test_continuous_runs() 221 dump_buf_if_failed(buf.c, sizeof(buf)); in test_continuous_runs() 242 g_assert_cmpfloat(calc_monobit_p(buf, sizeof(buf)), >, 0.01); in test_first_byte_monobit() 243 dump_buf_if_failed(buf, sizeof(buf)); in test_first_byte_monobit() 256 } buf; in test_first_byte_runs() local 267 g_assert_cmpfloat(calc_runs_p(buf.l, sizeof(buf) * BITS_PER_BYTE), >, 0.01); in test_first_byte_runs() [all …]
|
H A D | pnv-host-i2c-test.c | 152 buf[1] = 0; in pnv_i2c_pca9554_default_cfg() 157 buf[1] = 0xff; in pnv_i2c_pca9554_default_cfg() 162 buf[1] = 0xff; in pnv_i2c_pca9554_default_cfg() 246 buf[1] = 0xff; in pnv_i2c_pca9552_default_cfg() 249 buf[1] = 0x80; in pnv_i2c_pca9552_default_cfg() 252 buf[1] = 0xff; in pnv_i2c_pca9552_default_cfg() 255 buf[1] = 0x80; in pnv_i2c_pca9552_default_cfg() 260 buf[1] = 0x55; in pnv_i2c_pca9552_default_cfg() 263 buf[1] = 0x55; in pnv_i2c_pca9552_default_cfg() 266 buf[1] = 0x55; in pnv_i2c_pca9552_default_cfg() [all …]
|
/qemu/hw/scsi/ |
H A D | scsi-generic.c | 38 uint8_t *buf; member 195 memcpy(buf, r->buf, buf_used); in scsi_handle_inquiry_reply() 198 memcpy(r->buf + 8, buf + 8, buf_used - 8); in scsi_handle_inquiry_reply() 218 r->buf[page_idx] = r->buf[page_idx - 1]; in scsi_handle_inquiry_reply() 251 memcpy(r->buf, buf, MIN(r->buflen, len + 4)); in scsi_generic_emulate_block_limits() 395 s->blocksize = (r->buf[9] << 16) | (r->buf[10] << 8) | r->buf[11]; in scsi_write_complete() 570 memset(buf, 0, sizeof(buf)); in scsi_generic_set_vpd_bl_emulation() 606 memset(buf, 0, sizeof(buf)); in scsi_generic_read_device_identification() 618 len = MIN((buf[2] << 8) | buf[3], sizeof(buf) - 4); in scsi_generic_read_device_identification() 660 memset(buf, 0, sizeof(buf)); in get_stream_blocksize() [all …]
|
H A D | scsi-bus.c | 579 r->buf = g_byte_array_free(buf, FALSE); in scsi_target_emulate_report_luns() 1176 cmd->xfer = buf[4] | (buf[3] << 8); in scsi_req_xfer() 1182 cmd->xfer = buf[8] | (buf[7] << 8) | (buf[6] << 16); in scsi_req_xfer() 1231 cmd->xfer = buf[4] | (buf[3] << 8) | (buf[2] << 16); in scsi_req_stream_xfer() 1240 cmd->xfer = buf[14] | (buf[13] << 8) | (buf[12] << 16); in scsi_req_stream_xfer() 1250 cmd->xfer = buf[13] | (buf[12] << 8); in scsi_req_stream_xfer() 1270 cmd->xfer = buf[4] | (buf[3] << 8); in scsi_req_stream_xfer() 1291 cmd->xfer = buf[9] | (buf[8] << 8) | (buf[7] << 16); in scsi_req_medium_changer_xfer() 1315 cmd->xfer = buf[8] | (buf[7] << 8) | (buf[6] << 16); in scsi_req_scanner_length() 1420 memcpy(cmd->buf, buf, cmd->len); in scsi_req_parse_cdb() [all …]
|
/qemu/include/gdbstub/ |
H A D | helpers.h | 30 g_byte_array_append(buf, &val, 1); in gdb_get_reg8() 37 g_byte_array_append(buf, (uint8_t *) &to_word, 2); in gdb_get_reg16() 44 g_byte_array_append(buf, (uint8_t *) &to_long, 4); in gdb_get_reg32() 51 g_byte_array_append(buf, (uint8_t *) &to_quad, 8); in gdb_get_reg64() 61 g_byte_array_append(buf, (uint8_t *) &to_quad, 8); in gdb_get_reg128() 63 g_byte_array_append(buf, (uint8_t *) &to_quad, 8); in gdb_get_reg128() 66 g_byte_array_append(buf, (uint8_t *) &to_quad, 8); in gdb_get_reg128() 68 g_byte_array_append(buf, (uint8_t *) &to_quad, 8); in gdb_get_reg128() 92 return buf->data + buf->len - len; in gdb_get_reg_ptr() 96 #define gdb_get_regl(buf, val) gdb_get_reg64(buf, val) argument [all …]
|
/qemu/target/hexagon/ |
H A D | printinsn.c | 82 g_string_append(buf, "{"); in snprint_a_pkt_disas() 85 g_string_append(buf, "\t"); in snprint_a_pkt_disas() 86 snprintinsn(buf, &(pkt->insn[i])); in snprint_a_pkt_disas() 94 g_string_append(buf, "; "); in snprint_a_pkt_disas() 105 g_string_append(buf, " }"); in snprint_a_pkt_disas() 107 g_string_append(buf, " :endloop0"); in snprint_a_pkt_disas() 110 g_string_append(buf, " :endloop1"); in snprint_a_pkt_disas() 122 g_string_append(buf, "\n{\n"); in snprint_a_pkt_debug() 129 g_string_append(buf, "\t"); in snprint_a_pkt_debug() 130 snprintinsn(buf, &(pkt->insn[i])); in snprint_a_pkt_debug() [all …]
|
/qemu/util/ |
H A D | bufferiszero.c | 41 return (ldl_he_p(buf) | ldl_he_p(buf + len - 4)) == 0; in buffer_is_zero_int_lt256() 44 t = ldq_he_p(buf) | ldq_he_p(buf + len - 8); in buffer_is_zero_int_lt256() 45 p = QEMU_ALIGN_PTR_DOWN(buf + 8, 8); in buffer_is_zero_int_lt256() 46 e = QEMU_ALIGN_PTR_DOWN(buf + len - 1, 8); in buffer_is_zero_int_lt256() 61 uint64_t t = ldq_he_p(buf) | ldq_he_p(buf + len - 8); in buffer_is_zero_int_ge256() 94 buffer_zero_sse2(const void *buf, size_t len) in buffer_zero_sse2() argument 97 __m128i v = *(__m128i_u *)(buf); in buffer_zero_sse2() 140 buffer_zero_avx2(const void *buf, size_t len) in buffer_zero_avx2() argument 143 __m256i v = *(__m256i_u *)(buf); in buffer_zero_avx2() 219 t0 = vld1q_u32(buf) | vld1q_u32(buf + len - 16); in buffer_is_zero_simd() [all …]
|
H A D | unicode.c | 133 buf[0] = codepoint & 0x7F; in mod_utf8_encode() 134 buf[1] = 0; in mod_utf8_encode() 139 buf[1] = 0x80 | (codepoint & 0x3F); in mod_utf8_encode() 140 buf[2] = 0; in mod_utf8_encode() 146 buf[2] = 0x80 | (codepoint & 0x3F); in mod_utf8_encode() 147 buf[3] = 0; in mod_utf8_encode() 150 buf[0] = 0xF0 | ((codepoint >> 18) & 0x07); in mod_utf8_encode() 151 buf[1] = 0x80 | ((codepoint >> 12) & 0x3F); in mod_utf8_encode() 152 buf[2] = 0x80 | ((codepoint >> 6) & 0x3F); in mod_utf8_encode() 153 buf[3] = 0x80 | (codepoint & 0x3F); in mod_utf8_encode() [all …]
|
/qemu/tests/tcg/s390x/ |
H A D | lcbb.c | 35 test_lcbb(&buf[0], 0, 16, 0); in main() 36 test_lcbb(&buf[63], 0, 1, 3); in main() 37 test_lcbb(&buf[0], 1, 16, 0); in main() 38 test_lcbb(&buf[127], 1, 1, 3); in main() 39 test_lcbb(&buf[0], 2, 16, 0); in main() 40 test_lcbb(&buf[255], 2, 1, 3); in main() 41 test_lcbb(&buf[0], 3, 16, 0); in main() 42 test_lcbb(&buf[511], 3, 1, 3); in main() 43 test_lcbb(&buf[0], 4, 16, 0); in main() 44 test_lcbb(&buf[1023], 4, 1, 3); in main() [all …]
|
/qemu/hw/net/rocker/ |
H A D | rocker_tlv.h | 126 const RockerTlv *head = (const RockerTlv *) buf; in rocker_tlv_parse() 148 return (RockerTlv *) (buf + buf_pos); in rocker_tlv_start() 151 static inline void rocker_tlv_put_iov(char *buf, int *buf_pos, in rocker_tlv_put_iov() argument 159 tlv = rocker_tlv_start(buf, *buf_pos); in rocker_tlv_put_iov() 167 static inline void rocker_tlv_put(char *buf, int *buf_pos, in rocker_tlv_put() argument 175 rocker_tlv_put_iov(buf, buf_pos, type, &iov, 1); in rocker_tlv_put() 178 static inline void rocker_tlv_put_u8(char *buf, int *buf_pos, in rocker_tlv_put_u8() argument 184 static inline void rocker_tlv_put_u16(char *buf, int *buf_pos, in rocker_tlv_put_u16() argument 226 RockerTlv *start = rocker_tlv_start(buf, *buf_pos); in rocker_tlv_nest_start() 228 rocker_tlv_put(buf, buf_pos, type, 0, NULL); in rocker_tlv_nest_start() [all …]
|
/qemu/target/ppc/ |
H A D | gdbstub.c | 121 gdb_get_regl(buf, env->gpr[n]); in ppc_cpu_gdb_read_register() 125 gdb_get_regl(buf, env->nip); in ppc_cpu_gdb_read_register() 128 gdb_get_regl(buf, env->msr); in ppc_cpu_gdb_read_register() 133 gdb_get_reg32(buf, cr); in ppc_cpu_gdb_read_register() 137 gdb_get_regl(buf, env->lr); in ppc_cpu_gdb_read_register() 147 mem_buf = buf->data + buf->len - r; in ppc_cpu_gdb_read_register() 170 gdb_get_reg64(buf, n - 64); in ppc_cpu_gdb_read_register_apple() 171 gdb_get_reg64(buf, 0); in ppc_cpu_gdb_read_register_apple() 183 gdb_get_reg32(buf, cr); in ppc_cpu_gdb_read_register_apple() 200 mem_buf = buf->data + buf->len - r; in ppc_cpu_gdb_read_register_apple() [all …]
|
/qemu/tests/tcg/hexagon/ |
H A D | load_align.c | 44 buf[i] = i + 1; in init_buf() 138 checkp(ptr, &buf[0 * (SIZE)]); \ 141 checkp(ptr, &buf[1 * (SIZE)]); \ 144 checkp(ptr, &buf[2 * (SIZE)]); \ 147 checkp(ptr, &buf[3 * (SIZE)]); \ 177 void *ptr = buf; \ 220 void *ptr = buf; \ 255 void *ptr = buf; \ 258 checkp(ptr, &buf[1 * (INC)]); \ 299 void *ptr = buf; \ [all …]
|
H A D | load_unpack.c | 47 buf[i] = sign | (i + 1); in init_buf() 153 checkp(ptr, &buf[0 * (SIZE)]); \ 156 checkp(ptr, &buf[1 * (SIZE)]); \ 159 checkp(ptr, &buf[2 * (SIZE)]); \ 162 checkp(ptr, &buf[3 * (SIZE)]); \ 196 void *ptr = buf; \ 244 void *ptr = buf; \ 284 void *ptr = buf; \ 288 checkp(ptr, &buf[1 * (INC)]); \ 333 void *ptr = buf; \ [all …]
|
/qemu/hw/acpi/ |
H A D | aml-build.c | 454 var->buf = build_alloc_array(); in aml_alloc() 479 build_free_array(var->buf); in aml_free() 511 build_append_array(buf, child->buf); in aml_append() 529 build_append_byte(buf, 0); in aml_append() 532 build_buffer(buf, child->op); in aml_append() 540 build_append_array(parent_ctx->buf, buf); in aml_append() 541 build_free_array(buf); in aml_append() 579 build_append_int(var->buf, val); in aml_int() 1198 build_append_byte(var->buf, rs); in aml_operation_region() 1200 build_append_int(var->buf, len); in aml_operation_region() [all …]
|
/qemu/pc-bios/s390-ccw/ |
H A D | menu.c | 95 buf[--idx] = 0; in read_prompt() 112 *buf = 0; in read_prompt() 119 char buf[11]; in get_index() local 123 memset(buf, 0, sizeof(buf)); in get_index() 127 len = read_prompt(buf, sizeof(buf) - 1); in get_index() 143 return atoui(buf); in get_index() 184 char buf[len + 2]; in zipl_print_entry() local 187 buf[len] = '\n'; in zipl_print_entry() 188 buf[len + 1] = '\0'; in zipl_print_entry() 190 sclp_print(buf); in zipl_print_entry() [all …]
|
/qemu/linux-user/ |
H A D | uname.c | 79 int sys_uname(struct new_utsname *buf) in sys_uname() argument 92 memset(buf, 0, sizeof(*buf)); in sys_uname() 93 COPY_UTSNAME_FIELD(buf->sysname, uts_buf.sysname); in sys_uname() 95 COPY_UTSNAME_FIELD(buf->release, uts_buf.release); in sys_uname() 96 COPY_UTSNAME_FIELD(buf->version, uts_buf.version); in sys_uname() 97 COPY_UTSNAME_FIELD(buf->machine, uts_buf.machine); in sys_uname() 132 struct new_utsname buf; in get_osversion() local 140 if (sys_uname(&buf)) in get_osversion() 142 s = buf.release; in get_osversion() 155 struct new_utsname buf; in init_qemu_uname_release() local [all …]
|
H A D | gen-vdso.c | 31 fprintf(outf, " 0x%08tx,\n", loc - buf); in output_reloc() 64 unsigned char *buf; in main() local 119 buf = malloc(total_len); in main() 120 if (buf == NULL) { in main() 147 fprintf(outf, " 0x%02x,", buf[i]); in main() 156 if (buf[EI_MAG0] != ELFMAG0 || buf[EI_MAG1] != ELFMAG1 || in main() 157 buf[EI_MAG2] != ELFMAG2 || buf[EI_MAG3] != ELFMAG3) { in main() 161 switch (buf[EI_DATA]) { in main() 170 inf_name, buf[EI_DATA]); in main() 184 switch (buf[EI_CLASS]) { in main() [all …]
|
/qemu/hw/xen/ |
H A D | xen-host-pci-device.c | 67 rc = read(fd, &buf, sizeof(buf) - 1); in xen_host_pci_get_resource() 73 buf[rc] = 0; in xen_host_pci_get_resource() 75 s = buf; in xen_host_pci_get_resource() 155 rc = read(fd, &buf, sizeof(buf) - 1); in xen_host_pci_get_value() 162 buf[rc] = 0; in xen_host_pci_get_value() 194 struct stat buf; in xen_host_pci_dev_is_virtfn() local 198 return !stat(path, &buf); in xen_host_pci_dev_is_virtfn() 244 uint8_t buf; in xen_host_pci_get_byte() local 247 *p = buf; in xen_host_pci_get_byte() 254 uint16_t buf; in xen_host_pci_get_word() local [all …]
|
/qemu/scsi/ |
H A D | utils.c | 23 if ((buf[0] >> 5) == 0 && buf[4] == 0) { in scsi_data_cdb_xfer() 32 switch (buf[0] >> 5) { in scsi_cdb_xfer() 34 return buf[4]; in scsi_cdb_xfer() 49 uint8_t *buf = cmd->buf; in scsi_cmd_lba() local 52 switch (buf[0] >> 5) { in scsi_cmd_lba() 75 switch (buf[0] >> 5) { in scsi_cdb_length() 128 buf[0] = 0x70; in scsi_build_sense_buf() 129 buf[2] = sense.key; in scsi_build_sense_buf() 130 buf[7] = 10; in scsi_build_sense_buf() 135 buf[0] = 0x72; in scsi_build_sense_buf() [all …]
|
/qemu/tests/tcg/multiarch/ |
H A D | testthread.c | 11 void checked_write(int fd, const void *buf, size_t count) in checked_write() argument 13 ssize_t rc = write(fd, buf, count); in checked_write() 20 char buf[512]; in thread1_func() local 23 snprintf(buf, sizeof(buf), "thread1: %d %s\n", i, (char *)arg); in thread1_func() 24 checked_write(1, buf, strlen(buf)); in thread1_func() 33 char buf[512]; in thread2_func() local 35 snprintf(buf, sizeof(buf), "thread2: %d %s\n", i, (char *)arg); in thread2_func() 36 checked_write(1, buf, strlen(buf)); in thread2_func()
|
/qemu/hw/display/ |
H A D | artist.c | 436 if (dst >= buf->size || src >= buf->size) { in block_move() 439 artist_rop8(s, buf, dst, buf->data[src]); in block_move() 501 if ((x1 >= buf->width && x2 >= buf->width) || in draw_line() 502 (y1 >= buf->height && y2 >= buf->height)) { in draw_line() 700 if (startx >= buf->width || starty >= buf->height || in font_write16() 805 width = buf->width; in get_vram_offset() 829 artist_vram_write4(s, buf, get_vram_offset(s, buf, pos >> 2, posy), in vram_bit_write() 877 if (!buf->size) { in artist_vram_read() 1334 memory_region_set_dirty(&buf->mr, 0, buf->size); in artist_invalidate() 1365 buf->data = memory_region_get_ram_ptr(&buf->mr); in artist_create_buffer() [all …]
|
/qemu/hw/char/ |
H A D | spapr_vty.c | 19 uint8_t buf[VTERM_BUFSIZE]; member 51 dev->buf[dev->in++ % VTERM_BUFSIZE] = buf[i]; in vty_receive() 69 if (n > 0 && (buf[n - 1] == '\r') && in vty_getchars() 73 buf[n++] = dev->buf[dev->out++ % VTERM_BUFSIZE]; in vty_getchars() 112 uint8_t buf[16]; in h_put_term_char() local 123 *((uint64_t *)buf) = cpu_to_be64(char0_7); in h_put_term_char() 126 vty_putchars(sdev, buf, len); in h_put_term_char() 139 uint8_t buf[16]; in h_get_term_char() local 146 *len = vty_getchars(sdev, buf, sizeof(buf)); in h_get_term_char() 148 memset(buf + *len, 0, 16 - *len); in h_get_term_char() [all …]
|