Home
last modified time | relevance | path

Searched refs:buf (Results 76 – 100 of 784) sorted by relevance

12345678910>>...32

/qemu/crypto/
H A Drandom-platform.c67 int qcrypto_random_bytes(void *buf, in qcrypto_random_bytes() argument
72 if (!CryptGenRandom(hCryptProv, buflen, buf)) { in qcrypto_random_bytes()
81 ssize_t got = getrandom(buf, buflen, 0); in qcrypto_random_bytes()
87 buf += got; in qcrypto_random_bytes()
97 ssize_t got = read(fd, buf, buflen); in qcrypto_random_bytes()
103 buf += got; in qcrypto_random_bytes()
H A Dblockpriv.h88 uint8_t *buf,
93 uint8_t *buf,
97 bool (*has_format)(const uint8_t *buf,
107 uint8_t *buf,
116 uint8_t *buf,
123 uint8_t *buf,
130 uint8_t *buf,
/qemu/tests/tcg/cris/libc/
H A Dcheck_glibc_kernelversion.c20 char *buf = bufmem; \
39 buf[MIN (reslen, (ssize_t) sizeof (bufmem) - 1)] = '\0'; \
42 buf = uts.release; \
48 cp = buf; \
83 char *buf = bufmem; in main() local
90 cp = buf; in main()
H A Dcheck_openpf3.c24 struct stat buf; in main() local
36 if (stat (PREFIX "testfoo2.tmp", &buf) != 0 in main()
37 || !S_ISREG (buf.st_mode)) in main()
40 if (stat ("testfoo2.tmp", &buf) != 0 in main()
41 || !S_ISREG (buf.st_mode)) in main()
/qemu/system/
H A Ddatadir.c37 char *buf; in qemu_find_file() local
57 buf = g_strdup_printf("%s/%s%s", data_dir[i], subdir, name); in qemu_find_file()
58 if (access(buf, R_OK) == 0) { in qemu_find_file()
59 trace_load_file(name, buf); in qemu_find_file()
60 return buf; in qemu_find_file()
62 g_free(buf); in qemu_find_file()
/qemu/semihosting/
H A Dconsole.c58 static void console_read(void *opaque, const uint8_t *buf, int size) in console_read() argument
63 fifo8_push(&c->fifo, *buf++); in console_read()
93 int qemu_semihosting_console_read(CPUState *cs, void *buf, int len) in qemu_semihosting_console_read() argument
102 *(char *)(buf + ret) = fifo8_pop(&c->fifo); in qemu_semihosting_console_read()
109 int qemu_semihosting_console_write(void *buf, int len) in qemu_semihosting_console_write() argument
112 int r = qemu_chr_write_all(console.chr, (uint8_t *)buf, len); in qemu_semihosting_console_write()
115 return fwrite(buf, 1, len, stderr); in qemu_semihosting_console_write()
/qemu/include/sysemu/
H A Ddma.h83 void *buf, dma_addr_t len, in dma_memory_rw_relaxed() argument
88 buf, len, dir == DMA_DIRECTION_FROM_DEVICE); in dma_memory_rw_relaxed()
93 void *buf, dma_addr_t len) in dma_memory_read_relaxed() argument
95 return dma_memory_rw_relaxed(as, addr, buf, len, in dma_memory_read_relaxed()
102 const void *buf, in dma_memory_write_relaxed() argument
105 return dma_memory_rw_relaxed(as, addr, (void *)buf, len, in dma_memory_write_relaxed()
125 void *buf, dma_addr_t len, in dma_memory_rw() argument
130 return dma_memory_rw_relaxed(as, addr, buf, len, dir, attrs); in dma_memory_rw()
147 void *buf, dma_addr_t len, in dma_memory_read() argument
150 return dma_memory_rw(as, addr, buf, len, in dma_memory_read()
[all …]
/qemu/tests/tcg/s390x/
H A Dbranch-relative-long.c37 unsigned char *buf; in main() local
49 buf = mmap(NULL, length, PROT_READ | PROT_WRITE | PROT_EXEC, in main()
51 if (buf == MAP_FAILED) { in main()
56 memcpy(buf, br_r14, br_r14_end - br_r14); in main()
58 void (*code)(void) = (void *)(buf + 0x100000000); in main()
65 munmap(buf, length); in main()
/qemu/hw/char/
H A Dsclpconsole-lm.c48 uint8_t buf[SIZE_CONSOLE_BUFFER]; member
79 static void chr_read(void *opaque, const uint8_t *buf, int size) in chr_read() argument
85 if (*buf == '\r' || *buf == '\n') { in chr_read()
94 scon->buf[scon->length] = *buf; in chr_read()
99 qemu_chr_fe_write_all(&scon->chr, buf, size); in chr_read()
125 static int get_console_data(SCLPEvent *event, uint8_t *buf, size_t *size, in get_console_data() argument
138 ebcdic_put(buf, (char *)&cons->buf, len); in get_console_data()
199 static int write_console_data(SCLPEvent *event, const uint8_t *buf, int len) in write_console_data() argument
210 return qemu_chr_fe_write_all(&scon->chr, buf, len); in write_console_data()
299 VMSTATE_UINT8_ARRAY(buf, SCLPConsoleLM, SIZE_CONSOLE_BUFFER),
/qemu/host/include/i386/host/
H A Dbufferiszero.c.inc16 buffer_zero_sse2(const void *buf, size_t len)
19 __m128i v = *(__m128i_u *)(buf);
20 __m128i w = *(__m128i_u *)(buf + len - 16);
22 const __m128i *p = QEMU_ALIGN_PTR_DOWN(buf + 16, 16);
23 const __m128i *e = QEMU_ALIGN_PTR_DOWN(buf + len - 1, 16);
62 buffer_zero_avx2(const void *buf, size_t len)
65 __m256i v = *(__m256i_u *)(buf);
66 __m256i w = *(__m256i_u *)(buf + len - 32);
68 const __m256i *p = QEMU_ALIGN_PTR_DOWN(buf + 32, 32);
69 const __m256i *e = QEMU_ALIGN_PTR_DOWN(buf + len - 1, 32);
/qemu/include/scsi/
H A Dutils.h36 uint8_t buf[SCSI_CMD_BUF_SIZE]; member
49 int scsi_build_sense(uint8_t *buf, SCSISense sense);
51 int scsi_build_sense_buf(uint8_t *buf, size_t max_size, SCSISense sense,
130 uint8_t *buf, int len, bool fixed);
134 uint32_t scsi_data_cdb_xfer(uint8_t *buf);
135 uint32_t scsi_cdb_xfer(uint8_t *buf);
136 int scsi_cdb_length(uint8_t *buf);
/qemu/linux-user/
H A Dlinuxload.c72 retval = read(bprm->src.fd, bprm->buf, BPRM_BUF_SIZE); in prepare_binprm()
79 memset(bprm->buf + retval, 0, BPRM_BUF_SIZE - retval); in prepare_binprm()
82 bprm->src.cache = bprm->buf; in prepare_binprm()
159 if (bprm->buf[0] == 0x7f in loader_exec()
160 && bprm->buf[1] == 'E' in loader_exec()
161 && bprm->buf[2] == 'L' in loader_exec()
162 && bprm->buf[3] == 'F') { in loader_exec()
165 } else if (bprm->buf[0] == 'b' in loader_exec()
166 && bprm->buf[1] == 'F' in loader_exec()
167 && bprm->buf[2] == 'L' in loader_exec()
[all …]
/qemu/tests/multiboot/
H A Dmodules.c40 char buf[1024]; in test_main() local
47 if (size < sizeof(buf)) { in test_main()
48 memcpy(buf, (void*) mod->mod_start, size); in test_main()
49 buf[size - 1] = '\0'; in test_main()
50 printf(" Content: '%s'\n", buf); in test_main()
/qemu/include/hw/scsi/
H A Dscsi.h61 int (*parse_cdb)(SCSIDevice *dev, SCSICommand *cmd, uint8_t *buf,
64 uint8_t *buf, void *hba_private);
110 int cdrom_read_toc(int nb_sectors, uint8_t *buf, int msf, int start_track);
111 int cdrom_read_toc_raw(int nb_sectors, uint8_t *buf, int msf, int session_num);
118 int32_t (*send_command)(SCSIRequest *req, uint8_t *buf);
130 int (*parse_cdb)(SCSIDevice *dev, SCSICommand *cmd, uint8_t *buf,
210 uint8_t *buf, size_t buf_len, void *hba_private);
215 int scsi_bus_parse_cdb(SCSIDevice *dev, SCSICommand *cmd, uint8_t *buf,
217 int scsi_req_parse_cdb(SCSIDevice *dev, SCSICommand *cmd, uint8_t *buf,
226 int scsi_req_get_sense(SCSIRequest *req, uint8_t *buf, int len);
[all …]
/qemu/audio/
H A Dmixeng.c523 void mixeng_clear (struct st_sample *buf, int len) in mixeng_clear() argument
525 memset (buf, 0, len * sizeof (struct st_sample)); in mixeng_clear()
528 void mixeng_volume (struct st_sample *buf, int len, struct mixeng_volume *vol) in mixeng_volume() argument
531 mixeng_clear (buf, len); in mixeng_volume()
537 buf->l = buf->l * vol->l; in mixeng_volume()
538 buf->r = buf->r * vol->r; in mixeng_volume()
540 buf->l = (buf->l * vol->l) >> 32; in mixeng_volume()
541 buf->r = (buf->r * vol->r) >> 32; in mixeng_volume()
543 buf += 1; in mixeng_volume()
/qemu/target/s390x/
H A Dgdbstub.c71 static int cpu_read_ac_reg(CPUState *cs, GByteArray *buf, int n) in cpu_read_ac_reg() argument
78 return gdb_get_reg32(buf, env->aregs[n]); in cpu_read_ac_reg()
104 static int cpu_read_fp_reg(CPUState *cs, GByteArray *buf, int n) in cpu_read_fp_reg() argument
111 return gdb_get_reg32(buf, env->fpc); in cpu_read_fp_reg()
142 static int cpu_read_vreg(CPUState *cs, GByteArray *buf, int n) in cpu_read_vreg() argument
150 ret = gdb_get_reg64(buf, env->vregs[n][1]); in cpu_read_vreg()
153 ret = gdb_get_reg64(buf, env->vregs[n][0]); in cpu_read_vreg()
154 ret += gdb_get_reg64(buf, env->vregs[n][1]); in cpu_read_vreg()
186 static int cpu_read_c_reg(CPUState *cs, GByteArray *buf, int n) in cpu_read_c_reg() argument
193 return gdb_get_regl(buf, env->cregs[n]); in cpu_read_c_reg()
[all …]
/qemu/chardev/
H A Dchar-fe.c33 int qemu_chr_fe_write(CharBackend *be, const uint8_t *buf, int len) in qemu_chr_fe_write() argument
41 return qemu_chr_write(s, buf, len, false); in qemu_chr_fe_write()
44 int qemu_chr_fe_write_all(CharBackend *be, const uint8_t *buf, int len) in qemu_chr_fe_write_all() argument
52 return qemu_chr_write(s, buf, len, true); in qemu_chr_fe_write_all()
55 int qemu_chr_fe_read_all(CharBackend *be, uint8_t *buf, int len) in qemu_chr_fe_read_all() argument
66 return replay_char_read_all_load(buf); in qemu_chr_fe_read_all()
71 res = CHARDEV_GET_CLASS(s)->chr_sync_read(s, buf + offset, in qemu_chr_fe_read_all()
93 replay_char_read_all_save_buf(buf, offset); in qemu_chr_fe_read_all()
165 char buf[CHR_READ_BUF_LEN]; in qemu_chr_fe_printf() local
168 vsnprintf(buf, sizeof(buf), fmt, ap); in qemu_chr_fe_printf()
[all …]
/qemu/hw/s390x/
H A Ds390-stattrib.c120 uint8_t *buf; in cmma_load() local
131 buf = g_try_malloc(count); in cmma_load()
132 if (!buf) { in cmma_load()
138 qemu_get_buffer(f, buf, count); in cmma_load()
143 g_free(buf); in cmma_load()
205 uint8_t *buf; in cmma_save() local
210 buf = g_try_malloc(buflen); in cmma_save()
211 if (!buf) { in cmma_save()
219 g_free(buf); in cmma_save()
230 qemu_put_byte(f, buf[cx]); in cmma_save()
[all …]
/qemu/host/include/loongarch64/host/
H A Dbufferiszero.c.inc13 static bool buffer_is_zero_lsx(const void *buf, size_t len)
15 const void *p = QEMU_ALIGN_PTR_DOWN(buf + 16, 16);
17 const void *l = buf + len;
20 asm("vld $vr0,%2,0\n\t" /* first: buf + 0 */
21 "vld $vr1,%4,-16\n\t" /* last: buf + len - 16 */
63 : "r"(buf), "r"(e), "r"(l)
69 static bool buffer_is_zero_lasx(const void *buf, size_t len)
71 const void *p = QEMU_ALIGN_PTR_DOWN(buf + 32, 32);
73 const void *l = buf + len;
76 asm("xvld $xr0,%2,0\n\t" /* first: buf + 0 */
[all …]
/qemu/hw/scsi/
H A Dscsi-disk.c318 switch (cmd->buf[0]) { in scsi_is_cmd_fua()
601 if (r->req.cmd.buf[0] == VERIFY_10 || r->req.cmd.buf[0] == VERIFY_12 || in scsi_write_data()
1030 uint8_t *buf = r->req.cmd.buf; in scsi_get_event_status_notification() local
1885 uint8_t *buf; in scsi_disk_emulate_write_same() local
2280 command = buf[0]; in scsi_disk_dma_command()
2702 command = buf[0]; in scsi_new_request()
2720 uint8_t buf[36]; in get_device_type() local
2724 memset(buf, 0, sizeof(buf)); in get_device_type()
2729 buf, sizeof(buf), s->qdev.io_timeout); in get_device_type()
2734 if (buf[1] & 0x80) { in get_device_type()
[all …]
/qemu/hw/misc/
H A Dmos6522.c502 GString *buf = opaque; in qmp_x_query_via_foreach() local
512 g_string_append_printf(buf, " Registers:\n"); in qmp_x_query_via_foreach()
513 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
515 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
517 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
519 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
521 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
523 g_string_append_printf(buf, " %-*s: 0x%x\n", 4, in qmp_x_query_via_foreach()
546 g_string_append_printf(buf, " Timers:\n"); in qmp_x_query_via_foreach()
581 g_autoptr(GString) buf = g_string_new(""); in qmp_x_query_via()
[all …]
/qemu/block/
H A Dwin32-aio.c54 void *buf; member
86 iov_from_buf(qiov->iov, qiov->niov, 0, waiocb->buf, qiov->size); in win32_aio_process_completion()
88 qemu_vfree(waiocb->buf); in win32_aio_process_completion()
128 waiocb->buf = qemu_try_blockalign(bs, qiov->size); in win32_aio_submit()
129 if (waiocb->buf == NULL) { in win32_aio_submit()
133 iov_to_buf(qiov->iov, qiov->niov, 0, waiocb->buf, qiov->size); in win32_aio_submit()
137 waiocb->buf = qiov->iov[0].iov_base; in win32_aio_submit()
149 rc = ReadFile(hfile, waiocb->buf, waiocb->nbytes, NULL, &waiocb->ov); in win32_aio_submit()
151 rc = WriteFile(hfile, waiocb->buf, waiocb->nbytes, NULL, &waiocb->ov); in win32_aio_submit()
/qemu/util/
H A Dcacheflush.c29 SYSTEM_LOGICAL_PROCESSOR_INFORMATION *buf; in sys_cache_info() local
46 buf = g_new0(SYSTEM_LOGICAL_PROCESSOR_INFORMATION, n); in sys_cache_info()
47 if (!GetLogicalProcessorInformation(buf, &size)) { in sys_cache_info()
52 if (buf[i].Relationship == RelationCache in sys_cache_info()
53 && buf[i].Cache.Level == 1) { in sys_cache_info()
54 switch (buf[i].Cache.Type) { in sys_cache_info()
56 *isize = *dsize = buf[i].Cache.LineSize; in sys_cache_info()
59 *isize = buf[i].Cache.LineSize; in sys_cache_info()
62 *dsize = buf[i].Cache.LineSize; in sys_cache_info()
70 g_free(buf); in sys_cache_info()
/qemu/tests/qtest/
H A Dide-test.c332 uint8_t *buf; in test_bmdma_simple_rw() local
346 buf = g_malloc(len); in test_bmdma_simple_rw()
390 g_free(buf); in test_bmdma_simple_rw()
408 uint8_t *buf; in test_bmdma_trim() local
420 buf = g_malloc(len); in test_bmdma_trim()
446 g_free(buf); in test_bmdma_trim()
612 uint16_t buf[256]; in test_identify() local
700 void* buf; in make_dirty() local
705 buf = g_malloc(len); in make_dirty()
708 g_assert(buf); in make_dirty()
[all …]
/qemu/disas/
H A Dhexagon.c36 GString *buf; in print_insn_hexagon() local
60 buf = g_string_sized_new(PACKET_BUFFER_LEN); in print_insn_hexagon()
61 len = disassemble_hexagon(words, i, memaddr, buf); in print_insn_hexagon()
62 (*info->fprintf_func)(info->stream, "%s", buf->str); in print_insn_hexagon()
63 g_string_free(buf, true); in print_insn_hexagon()

12345678910>>...32