Home
last modified time | relevance | path

Searched refs:buf (Results 1 – 25 of 748) sorted by relevance

12345678910>>...30

/qemu/hw/ide/
H A Datapi.c76 buf[0] = 0x00; in cd_data_to_raw()
78 buf[11] = 0x00; in cd_data_to_raw()
79 buf += 12; in cd_data_to_raw()
83 buf += 4; in cd_data_to_raw()
85 buf += 2048; in cd_data_to_raw()
154 void *buf; in cd_read_sector() local
596 buf[6] = 0; in event_status_media()
597 buf[7] = 0; in event_status_media()
818 if (buf[2] != 0 || buf[3] != 0) { in cmd_get_configuration()
1012 nb_sectors = (buf[6] << 16) | (buf[7] << 8) | buf[8]; in cmd_read_cd()
[all …]
/qemu/contrib/vhost-user-gpu/
H A Dvugbm.c16 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 Dmonitor.c24 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 Dnpcm7xx_rng-test.c137 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 Dpnv-host-i2c-test.c152 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 Dscsi-generic.c38 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 Dscsi-bus.c579 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 Dhelpers.h30 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 Dprintinsn.c82 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 Dbufferiszero.c41 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 Dunicode.c133 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 Dlcbb.c35 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 Drocker_tlv.h126 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 Dgdbstub.c121 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 Dload_align.c44 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 Dload_unpack.c47 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 Daml-build.c454 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 Dmenu.c95 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 Duname.c79 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 Dgen-vdso.c31 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 Dxen-host-pci-device.c67 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 Dutils.c23 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 Dtestthread.c11 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 Dartist.c436 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 Dspapr_vty.c19 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 …]

12345678910>>...30