1 project('qemu', ['c'], meson_version: '>=0.63.0',
2 default_options: ['warning_level=1', 'c_std=gnu11', 'cpp_std=gnu++11', 'b_colorout=auto',
3 'b_staticpic=false', 'stdsplit=false', 'optimization=2', 'b_pie=true'],
4 version: files('VERSION'))
6 add_test_setup('quick', exclude_suites: ['slow', 'thorough'], is_default: true)
7 add_test_setup('slow', exclude_suites: ['thorough'], env: ['G_TEST_SLOW=1', 'SPEED=slow'])
8 add_test_setup('thorough', env: ['G_TEST_SLOW=1', 'SPEED=thorough'])
10 meson.add_postconf_script(find_program('scripts/symlink-install-tree.py'))
12 not_found = dependency('', required: false)
13 keyval = import('keyval')
14 ss = import('sourceset')
17 targetos = host_machine.system()
18 sh = find_program('sh')
19 config_host = keyval.load(meson.current_build_dir() / 'config-host.mak')
21 cc = meson.get_compiler('c')
23 if targetos == 'windows' and add_languages('cpp', required: false, native: false)
24 all_languages += ['cpp']
25 cxx = meson.get_compiler('cpp')
27 if targetos == 'darwin' and \
28 add_languages('objc', required: get_option('cocoa'), native: false)
29 all_languages += ['objc']
30 objc = meson.get_compiler('objc')
33 # Temporary directory used for files created while
34 # configure runs. Since it is in the build directory
35 # we can safely blow away any previous version of it
36 # (and we need not jump through hoops to try to delete
37 # it when configure exits.)
38 tmpdir = meson.current_build_dir() / 'meson-private/temp'
40 if get_option('qemu_suffix').startswith('/')
41 error('qemu_suffix cannot start with a /')
44 qemu_confdir = get_option('sysconfdir') / get_option('qemu_suffix')
45 qemu_datadir = get_option('datadir') / get_option('qemu_suffix')
46 qemu_docdir = get_option('docdir') / get_option('qemu_suffix')
47 qemu_moddir = get_option('libdir') / get_option('qemu_suffix')
49 qemu_desktopdir = get_option('datadir') / 'applications'
50 qemu_icondir = get_option('datadir') / 'icons'
52 config_host_data = configuration_data()
54 qapi_trace_events = []
56 bsd_oses = ['gnu/kfreebsd', 'freebsd', 'netbsd', 'openbsd', 'dragonfly', 'darwin']
57 supported_oses = ['windows', 'freebsd', 'netbsd', 'openbsd', 'darwin', 'sunos', 'linux']
58 supported_cpus = ['ppc', 'ppc64', 's390x', 'riscv32', 'riscv64', 'x86', 'x86_64',
59 'arm', 'aarch64', 'loongarch64', 'mips', 'mips64', 'sparc64']
61 cpu = host_machine.cpu_family()
63 target_dirs = config_host['TARGET_DIRS'].split()
64 have_linux_user = false
67 foreach target : target_dirs
68 have_linux_user = have_linux_user or target.endswith('linux-user')
69 have_bsd_user = have_bsd_user or target.endswith('bsd-user')
70 have_system = have_system or target.endswith('-softmmu')
72 have_user = have_linux_user or have_bsd_user
73 have_tools = get_option('tools') \
74 .disable_auto_if(not have_system) \
76 have_ga = get_option('guest_agent') \
77 .disable_auto_if(not have_system and not have_tools) \
78 .require(targetos in ['sunos', 'linux', 'windows', 'freebsd', 'netbsd', 'openbsd'],
79 error_message: 'unsupported OS for QEMU guest agent') \
81 enable_modules = get_option('modules') \
82 .require(targetos != 'windows',
83 error_message: 'Modules are not available for Windows') \
84 .require(not get_option('prefer_static'),
85 error_message: 'Modules are incompatible with static linking') \
87 have_block = have_system or have_tools
89 python = import('python').find_installation()
91 if cpu not in supported_cpus
97 elif cpu in ['riscv32', 'riscv64']
103 if cpu in ['x86', 'x86_64']
104 kvm_targets = ['i386-softmmu', 'x86_64-softmmu']
105 elif cpu == 'aarch64'
106 kvm_targets = ['aarch64-softmmu']
108 kvm_targets = ['s390x-softmmu']
109 elif cpu in ['ppc', 'ppc64']
110 kvm_targets = ['ppc-softmmu', 'ppc64-softmmu']
111 elif cpu in ['mips', 'mips64']
112 kvm_targets = ['mips-softmmu', 'mipsel-softmmu', 'mips64-softmmu', 'mips64el-softmmu']
113 elif cpu in ['riscv32']
114 kvm_targets = ['riscv32-softmmu']
115 elif cpu in ['riscv64']
116 kvm_targets = ['riscv64-softmmu']
122 if get_option('kvm').allowed() and targetos == 'linux'
123 kvm_targets_c = '"' + '" ,"'.join(kvm_targets) + '"'
125 config_host_data.set('CONFIG_KVM_TARGETS', kvm_targets_c)
127 accelerator_targets = { 'CONFIG_KVM': kvm_targets }
129 if cpu in ['aarch64']
130 accelerator_targets += {
131 'CONFIG_HVF': ['aarch64-softmmu']
135 if cpu in ['x86', 'x86_64', 'arm', 'aarch64']
136 # i386 emulator provides xenpv machine type for multiple architectures
137 accelerator_targets += {
138 'CONFIG_XEN': ['i386-softmmu', 'x86_64-softmmu', 'aarch64-softmmu'],
141 if cpu in ['x86', 'x86_64']
142 accelerator_targets += {
143 'CONFIG_HVF': ['x86_64-softmmu'],
144 'CONFIG_NVMM': ['i386-softmmu', 'x86_64-softmmu'],
145 'CONFIG_WHPX': ['i386-softmmu', 'x86_64-softmmu'],
150 # Darwin does not support references to thread-local variables in modules
151 if targetos != 'darwin'
152 modular_tcg = ['i386-softmmu', 'x86_64-softmmu']
155 edk2_targets = [ 'arm-softmmu', 'aarch64-softmmu', 'i386-softmmu', 'x86_64-softmmu' ]
156 unpack_edk2_blobs = false
157 foreach target : edk2_targets
158 if target in target_dirs
159 bzip2 = find_program('bzip2', required: get_option('install_blobs'))
160 unpack_edk2_blobs = bzip2.found()
167 if 'dtrace' in get_option('trace_backends')
168 dtrace = find_program('dtrace', required: true)
169 stap = find_program('stap', required: false)
171 # Workaround to avoid dtrace(1) producing a file with 'hidden' symbol
172 # visibility. Define STAP_SDT_V2 to produce 'default' symbol visibility
173 # instead. QEMU --enable-modules depends on this because the SystemTap
174 # semaphores are linked into the main binary and not the module's shared
176 add_global_arguments('-DSTAP_SDT_V2',
177 native: false, language: all_languages)
181 if get_option('iasl') == ''
182 iasl = find_program('iasl', required: false)
184 iasl = find_program(get_option('iasl'), required: true)
191 foreach lang : all_languages
192 compiler = meson.get_compiler(lang)
193 if compiler.get_id() == 'gcc' and compiler.version().version_compare('>=7.4')
195 elif compiler.get_id() == 'clang' and compiler.compiles('''
196 #ifdef __apple_build_version__
197 # if __clang_major__ < 12 || (__clang_major__ == 12 && __clang_minor__ < 0)
198 # error You need at least XCode Clang v12.0 to compile QEMU
201 # if __clang_major__ < 10 || (__clang_major__ == 10 && __clang_minor__ < 0)
202 # error You need at least Clang v10.0 to compile QEMU
207 error('You either need GCC v7.4 or Clang v10.0 (or XCode Clang v12.0) to compile QEMU')
211 # default flags for all hosts
212 # We use -fwrapv to tell the compiler that we require a C dialect where
213 # left shift of signed integers is well defined and has the expected
214 # 2s-complement style results. (Both clang and gcc agree that it
215 # provides these semantics.)
217 qemu_common_flags = [
218 '-D_GNU_SOURCE', '-D_FILE_OFFSET_BITS=64', '-D_LARGEFILE_SOURCE',
219 '-fno-strict-aliasing', '-fno-common', '-fwrapv' ]
223 if targetos == 'darwin'
224 # Disable attempts to use ObjectiveC features in os/object.h since they
225 # won't work when we're compiling with gcc as a C compiler.
226 qemu_common_flags += '-DOS_OBJECT_USE_OBJC=0'
227 elif targetos == 'solaris'
228 # needed for CMSG_ macros in sys/socket.h
229 qemu_common_flags += '-D_XOPEN_SOURCE=600'
230 # needed for TIOCWIN* defines in termios.h
231 qemu_common_flags += '-D__EXTENSIONS__'
232 elif targetos == 'haiku'
233 qemu_common_flags += ['-DB_USE_POSITIVE_POSIX_ERRORS', '-D_BSD_SOURCE', '-fPIC']
236 # __sync_fetch_and_and requires at least -march=i486. Many toolchains
237 # use i686 as default anyway, but for those that don't, an explicit
238 # specification is necessary
239 if host_arch == 'i386' and not cc.links('''
240 static int sfaa(int *ptr)
242 return __sync_fetch_and_and(ptr, 0);
248 val = __sync_val_compare_and_swap(&val, 0, 1);
252 qemu_common_flags = ['-march=i486'] + qemu_common_flags
255 if get_option('gprof')
256 qemu_common_flags += ['-p']
257 qemu_ldflags += ['-p']
260 if get_option('prefer_static')
261 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static'
264 # Meson currently only handles pie as a boolean for now, so if the user
265 # has explicitly disabled PIE we need to extend our cflags.
267 # -no-pie is supposedly a linker flag that has no effect on the compiler
268 # command line, but some distros, that didn't quite know what they were
269 # doing, made local changes to gcc's specs file that turned it into
270 # a compiler command-line flag.
272 # What about linker flags? For a static build, no PIE is implied by -static
273 # which we added above (and if it's not because of the same specs patching,
274 # there's nothing we can do: compilation will fail, report a bug to your
275 # distro and do not use --disable-pie in the meanwhile). For dynamic linking,
276 # instead, we can't add -no-pie because it overrides -shared: the linker then
277 # tries to build an executable instead of a shared library and fails. So
278 # don't add -no-pie anywhere and cross fingers. :(
279 if not get_option('b_pie')
280 qemu_common_flags += cc.get_supported_arguments('-fno-pie', '-no-pie')
283 if not get_option('stack_protector').disabled()
284 stack_protector_probe = '''
285 int main(int argc, char *argv[])
287 char arr[64], *p = arr, *c = argv[argc - 1];
293 have_stack_protector = false
294 foreach arg : ['-fstack-protector-strong', '-fstack-protector-all']
295 # We need to check both a compile and a link, since some compiler
296 # setups fail only on a .c->.o compile and some only at link time
297 if cc.compiles(stack_protector_probe, args: ['-Werror', arg]) and \
298 cc.links(stack_protector_probe, args: ['-Werror', arg])
299 have_stack_protector = true
305 get_option('stack_protector') \
306 .require(have_stack_protector, error_message: 'Stack protector not supported')
309 coroutine_backend = get_option('coroutine_backend')
311 #include <ucontext.h>
312 #ifdef __stub_makecontext
313 #error Ignoring glibc stub makecontext which will always fail
315 int main(void) { makecontext(0, 0, 0); return 0; }'''
317 # On Windows the only valid backend is the Windows specific one.
318 # For POSIX prefer ucontext, but it's not always possible. The fallback
320 supported_backends = []
321 if targetos == 'windows'
322 supported_backends += ['windows']
324 if targetos != 'darwin' and cc.links(ucontext_probe)
325 supported_backends += ['ucontext']
327 supported_backends += ['sigaltstack']
330 if coroutine_backend == 'auto'
331 coroutine_backend = supported_backends[0]
332 elif coroutine_backend not in supported_backends
333 error('"@0@" backend requested but not available. Available backends: @1@' \
334 .format(coroutine_backend, ', '.join(supported_backends)))
337 # Compiles if SafeStack *not* enabled
338 safe_stack_probe = '''
341 #if defined(__has_feature)
342 #if __has_feature(safe_stack)
343 #error SafeStack Enabled
348 if get_option('safe_stack') != not cc.compiles(safe_stack_probe)
349 safe_stack_arg = get_option('safe_stack') ? '-fsanitize=safe-stack' : '-fno-sanitize=safe-stack'
350 if get_option('safe_stack') != not cc.compiles(safe_stack_probe, args: safe_stack_arg)
351 error(get_option('safe_stack') \
352 ? 'SafeStack not supported by your compiler' \
353 : 'Cannot disable SafeStack')
355 qemu_cflags += safe_stack_arg
356 qemu_ldflags += safe_stack_arg
358 if get_option('safe_stack') and coroutine_backend != 'ucontext'
359 error('SafeStack is only supported with the ucontext coroutine backend')
362 if get_option('sanitizers')
363 if cc.has_argument('-fsanitize=address')
364 qemu_cflags = ['-fsanitize=address'] + qemu_cflags
365 qemu_ldflags = ['-fsanitize=address'] + qemu_ldflags
368 # Detect static linking issue with ubsan - https://gcc.gnu.org/bugzilla/show_bug.cgi?id=84285
369 if cc.links('int main(int argc, char **argv) { return argc + 1; }',
370 args: [qemu_ldflags, '-fsanitize=undefined'])
371 qemu_cflags = ['-fsanitize=undefined'] + qemu_cflags
372 qemu_ldflags = ['-fsanitize=undefined'] + qemu_ldflags
376 # Thread sanitizer is, for now, much noisier than the other sanitizers;
377 # keep it separate until that is not the case.
378 if get_option('tsan')
379 if get_option('sanitizers')
380 error('TSAN is not supported with other sanitizers')
382 if not cc.has_function('__tsan_create_fiber',
383 args: '-fsanitize=thread',
384 prefix: '#include <sanitizer/tsan_interface.h>')
385 error('Cannot enable TSAN due to missing fiber annotation interface')
387 qemu_cflags = ['-fsanitize=thread'] + qemu_cflags
388 qemu_ldflags = ['-fsanitize=thread'] + qemu_ldflags
391 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
392 # The combination is known as "full relro", because .got.plt is read-only too.
393 qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now')
395 if targetos == 'windows'
396 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--no-seh', '-Wl,--nxcompat')
397 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--dynamicbase', '-Wl,--high-entropy-va')
400 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
401 if targetos != 'sunos' and not get_option('tsan')
402 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--warn-common')
405 if get_option('fuzzing')
406 # Specify a filter to only instrument code that is directly related to
408 configure_file(output: 'instrumentation-filter',
409 input: 'scripts/oss-fuzz/instrumentation-filter-template',
412 if cc.compiles('int main () { return 0; }',
413 name: '-fsanitize-coverage-allowlist=/dev/null',
414 args: ['-fsanitize-coverage-allowlist=/dev/null',
415 '-fsanitize-coverage=trace-pc'] )
416 qemu_common_flags += ['-fsanitize-coverage-allowlist=instrumentation-filter']
419 if get_option('fuzzing_engine') == ''
420 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the
421 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link
422 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be
423 # unable to bind the fuzzer-related callbacks added by instrumentation.
424 qemu_common_flags += ['-fsanitize=fuzzer-no-link']
425 qemu_ldflags += ['-fsanitize=fuzzer-no-link']
426 # For the actual fuzzer binaries, we need to link against the libfuzzer
427 # library. They need to be configurable, to support OSS-Fuzz
428 fuzz_exe_ldflags = ['-fsanitize=fuzzer']
430 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and
431 # the needed CFLAGS have already been provided
432 fuzz_exe_ldflags = get_option('fuzzing_engine').split()
436 add_global_arguments(qemu_common_flags, native: false, language: all_languages)
437 add_global_link_arguments(qemu_ldflags, native: false, language: all_languages)
439 # Collect warnings that we want to enable
444 '-Wmissing-prototypes',
445 '-Wstrict-prototypes',
447 '-Wold-style-declaration',
448 '-Wold-style-definition',
453 '-Wignored-qualifiers',
457 '-Wexpansion-to-defined',
458 '-Wimplicit-fallthrough=2',
459 '-Wmissing-format-attribute',
460 '-Wno-initializer-overrides',
461 '-Wno-missing-include-dirs',
462 '-Wno-shift-negative-value',
463 '-Wno-string-plus-int',
464 '-Wno-typedef-redefinition',
465 '-Wno-tautological-type-limit-compare',
467 '-Wno-gnu-variable-sized-type-not-at-end',
470 if targetos != 'darwin'
471 warn_flags += ['-Wthread-safety']
474 # Set up C++ compiler flags
476 if 'cpp' in all_languages
477 qemu_cxxflags = ['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'] + qemu_cflags
480 # clang does not support glibc + FORTIFY_SOURCE (is it still true?)
481 if get_option('optimization') != '0' and targetos == 'linux'
482 if cc.get_id() == 'gcc'
483 qemu_cflags += ['-U_FORTIFY_SOURCE', '-D_FORTIFY_SOURCE=2']
485 if 'cpp' in all_languages and cxx.get_id() == 'gcc'
486 qemu_cxxflags += ['-U_FORTIFY_SOURCE', '-D_FORTIFY_SOURCE=2']
490 add_project_arguments(qemu_cflags, native: false, language: 'c')
491 add_project_arguments(cc.get_supported_arguments(warn_flags), native: false, language: 'c')
492 if 'cpp' in all_languages
493 add_project_arguments(qemu_cxxflags, native: false, language: 'cpp')
494 add_project_arguments(cxx.get_supported_arguments(warn_flags), native: false, language: 'cpp')
496 if 'objc' in all_languages
497 # Note sanitizer flags are not applied to Objective-C sources!
498 add_project_arguments(objc.get_supported_arguments(warn_flags), native: false, language: 'objc')
500 if targetos == 'linux'
501 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers',
502 '-isystem', 'linux-headers',
503 language: all_languages)
506 add_project_arguments('-iquote', '.',
507 '-iquote', meson.current_source_dir(),
508 '-iquote', meson.current_source_dir() / 'include',
509 language: all_languages)
511 # If a host-specific include directory exists, list that first...
512 host_include = meson.current_source_dir() / 'host/include/'
513 if fs.is_dir(host_include / host_arch)
514 add_project_arguments('-iquote', host_include / host_arch,
515 language: all_languages)
517 # ... followed by the generic fallback.
518 add_project_arguments('-iquote', host_include / 'generic',
519 language: all_languages)
521 sparse = find_program('cgcc', required: get_option('sparse'))
524 command: [find_program('scripts/check_sparse.py'),
525 'compile_commands.json', sparse.full_path(), '-Wbitwise',
526 '-Wno-transparent-union', '-Wno-old-initializer',
527 '-Wno-non-pointer-null'])
530 ###########################################
531 # Target-specific checks and dependencies #
532 ###########################################
535 if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \
538 #include <sys/types.h>
539 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
540 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
542 args: ['-Werror', '-fsanitize=fuzzer'])
543 error('Your compiler does not support -fsanitize=fuzzer')
547 if 'ftrace' in get_option('trace_backends') and targetos != 'linux'
548 error('ftrace is supported only on Linux')
550 if 'syslog' in get_option('trace_backends') and not cc.compiles('''
553 openlog("qemu", LOG_PID, LOG_DAEMON);
554 syslog(LOG_INFO, "configure");
557 error('syslog is not supported on this system')
560 # Miscellaneous Linux-only features
561 get_option('mpath') \
562 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux')
564 multiprocess_allowed = get_option('multiprocess') \
565 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \
568 vfio_user_server_allowed = get_option('vfio_user_server') \
569 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \
572 have_tpm = get_option('tpm') \
573 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \
577 have_vhost_user = get_option('vhost_user') \
578 .disable_auto_if(targetos != 'linux') \
579 .require(targetos != 'windows',
580 error_message: 'vhost-user is not available on Windows').allowed()
581 have_vhost_vdpa = get_option('vhost_vdpa') \
582 .require(targetos == 'linux',
583 error_message: 'vhost-vdpa is only available on Linux').allowed()
584 have_vhost_kernel = get_option('vhost_kernel') \
585 .require(targetos == 'linux',
586 error_message: 'vhost-kernel is only available on Linux').allowed()
587 have_vhost_user_crypto = get_option('vhost_crypto') \
588 .require(have_vhost_user,
589 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed()
591 have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel
593 have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed()
594 have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed()
595 have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed()
596 have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa
598 # Target-specific libraries and flags
599 libm = cc.find_library('m', required: false)
600 threads = dependency('threads')
601 util = cc.find_library('util', required: false)
607 emulator_link_args = []
614 if targetos == 'windows'
615 midl = find_program('midl', required: false)
616 widl = find_program('widl', required: false)
617 pathcch = cc.find_library('pathcch')
618 socket = cc.find_library('ws2_32')
619 winmm = cc.find_library('winmm')
621 win = import('windows')
622 version_res = win.compile_resources('version.rc',
623 depend_files: files('pc-bios/qemu-nsis.ico'),
624 include_directories: include_directories('.'))
626 elif targetos == 'darwin'
627 coref = dependency('appleframeworks', modules: 'CoreFoundation')
628 iokit = dependency('appleframeworks', modules: 'IOKit', required: false)
629 host_dsosuf = '.dylib'
630 elif targetos == 'sunos'
631 socket = [cc.find_library('socket'),
632 cc.find_library('nsl'),
633 cc.find_library('resolv')]
634 elif targetos == 'haiku'
635 socket = [cc.find_library('posix_error_mapper'),
636 cc.find_library('network'),
637 cc.find_library('bsd')]
638 elif targetos == 'openbsd'
639 if get_option('tcg').allowed() and target_dirs.length() > 0
640 # Disable OpenBSD W^X if available
641 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded')
645 # Target-specific configuration of accelerators
647 if get_option('kvm').allowed() and targetos == 'linux'
648 accelerators += 'CONFIG_KVM'
650 if get_option('whpx').allowed() and targetos == 'windows'
651 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64'
652 error('WHPX requires 64-bit host')
653 elif cc.has_header('winhvplatform.h', required: get_option('whpx')) and \
654 cc.has_header('winhvemulation.h', required: get_option('whpx'))
655 accelerators += 'CONFIG_WHPX'
658 if get_option('hvf').allowed()
659 hvf = dependency('appleframeworks', modules: 'Hypervisor',
660 required: get_option('hvf'))
662 accelerators += 'CONFIG_HVF'
665 if targetos == 'netbsd'
666 nvmm = cc.find_library('nvmm', required: get_option('nvmm'))
668 accelerators += 'CONFIG_NVMM'
673 if get_option('tcg').allowed()
674 if host_arch == 'unknown'
675 if get_option('tcg_interpreter')
676 warning('Unsupported CPU @0@, will use TCG with TCI (slow)'.format(cpu))
678 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu))
680 elif get_option('tcg_interpreter')
681 warning('Use of the TCG interpreter is not recommended on this host')
682 warning('architecture. There is a native TCG execution backend available')
683 warning('which provides substantially better performance and reliability.')
684 warning('It is strongly recommended to remove the --enable-tcg-interpreter')
685 warning('configuration option on this architecture to use the native')
688 if get_option('tcg_interpreter')
690 config_host += { 'CONFIG_TCG_INTERPRETER': 'y' }
691 elif host_arch == 'x86_64'
693 elif host_arch == 'ppc64'
696 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch,
697 language: all_languages)
699 accelerators += 'CONFIG_TCG'
700 config_host += { 'CONFIG_TCG': 'y' }
703 if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled()
704 error('KVM not available on this platform')
706 if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled()
707 error('HVF not available on this platform')
709 if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled()
710 error('NVMM not available on this platform')
712 if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled()
713 error('WHPX not available on this platform')
720 # When bumping glib minimum version, please check also whether to increase
721 # the _WIN32_WINNT setting in osdep.h according to the value from glib
722 glib_req_ver = '>=2.56.0'
723 glib_pc = dependency('glib-2.0', version: glib_req_ver, required: true,
724 method: 'pkg-config')
727 gmodule = dependency('gmodule-export-2.0', version: glib_req_ver, required: true,
728 method: 'pkg-config')
729 elif config_host.has_key('CONFIG_PLUGIN')
730 gmodule = dependency('gmodule-no-export-2.0', version: glib_req_ver, required: true,
731 method: 'pkg-config')
736 # This workaround is required due to a bug in pkg-config file for glib as it
737 # doesn't define GLIB_STATIC_COMPILATION for pkg-config --static
738 if targetos == 'windows' and get_option('prefer_static')
739 glib_cflags += ['-DGLIB_STATIC_COMPILATION']
742 # Sanity check that the current size_t matches the
743 # size that glib thinks it should be. This catches
744 # problems on multi-arch where people try to build
745 # 32-bit QEMU while pointing at 64-bit glib headers
747 if not cc.compiles('''
751 #define QEMU_BUILD_BUG_ON(x) \
752 typedef char qemu_build_bug_on[(x)?-1:1] __attribute__((unused));
755 QEMU_BUILD_BUG_ON(sizeof(size_t) != GLIB_SIZEOF_SIZE_T);
757 }''', dependencies: glib_pc, args: glib_cflags)
758 error('''sizeof(size_t) doesn't match GLIB_SIZEOF_SIZE_T.
759 You probably need to set PKG_CONFIG_LIBDIR" to point
760 to the right pkg-config files for your build target.''')
763 # Silence clang warnings triggered by glib < 2.57.2
764 if not cc.compiles('''
769 static void foo_free(Foo *f)
773 G_DEFINE_AUTOPTR_CLEANUP_FUNC(Foo, foo_free)
774 int main(void) { return 0; }''', dependencies: glib_pc, args: ['-Wunused-function', '-Werror'])
775 glib_cflags += cc.get_supported_arguments('-Wno-unused-function')
777 glib = declare_dependency(dependencies: [glib_pc, gmodule],
778 compile_args: glib_cflags,
779 version: glib_pc.version())
781 # Check whether glib has gslice, which we have to avoid for correctness.
782 # TODO: remove this check and the corresponding workaround (qtree) when
783 # the minimum supported glib is >= 2.75.3
784 glib_has_gslice = glib.version().version_compare('<2.75.3')
786 # override glib dep to include the above refinements
787 meson.override_dependency('glib-2.0', glib)
789 # The path to glib.h is added to all compilation commands.
790 add_project_dependencies(glib.partial_dependency(compile_args: true, includes: true),
791 native: false, language: all_languages)
794 gdbus_codegen = not_found
795 gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio'
796 if not get_option('gio').auto() or have_system
797 gio = dependency('gio-2.0', required: get_option('gio'),
798 method: 'pkg-config')
799 if gio.found() and not cc.links('''
803 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
805 }''', dependencies: [glib, gio])
806 if get_option('gio').enabled()
807 error('The installed libgio is broken for static linking')
812 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'),
813 required: get_option('gio'))
814 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'),
815 method: 'pkg-config')
816 gio = declare_dependency(dependencies: [gio, gio_unix],
817 version: gio.version())
820 if gdbus_codegen.found() and get_option('cfi')
821 gdbus_codegen = not_found
822 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity'
825 xml_pp = find_program('scripts/xml-preprocess.py')
828 if 'ust' in get_option('trace_backends')
829 lttng = dependency('lttng-ust', required: true, version: '>= 2.1',
830 method: 'pkg-config')
833 if have_system or have_tools
834 pixman = dependency('pixman-1', required: have_system, version:'>=0.21.8',
835 method: 'pkg-config')
837 zlib = dependency('zlib', required: true)
840 if not get_option('linux_aio').auto() or have_block
841 libaio = cc.find_library('aio', has_headers: ['libaio.h'],
842 required: get_option('linux_aio'))
845 linux_io_uring_test = '''
846 #include <liburing.h>
847 #include <linux/errqueue.h>
849 int main(void) { return 0; }'''
851 linux_io_uring = not_found
852 if not get_option('linux_io_uring').auto() or have_block
853 linux_io_uring = dependency('liburing', version: '>=0.3',
854 required: get_option('linux_io_uring'),
855 method: 'pkg-config')
856 if not cc.links(linux_io_uring_test)
857 linux_io_uring = not_found
862 if not get_option('libnfs').auto() or have_block
863 libnfs = dependency('libnfs', version: '>=1.9.3',
864 required: get_option('libnfs'),
865 method: 'pkg-config')
870 #include <sys/types.h>
871 #ifdef CONFIG_LIBATTR
872 #include <attr/xattr.h>
874 #include <sys/xattr.h>
876 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }'''
879 have_old_libattr = false
880 if get_option('attr').allowed()
881 if cc.links(libattr_test)
882 libattr = declare_dependency()
884 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'],
885 required: get_option('attr'))
886 if libattr.found() and not \
887 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR')
889 if get_option('attr').enabled()
890 error('could not link libattr')
892 warning('could not link libattr, disabling')
895 have_old_libattr = libattr.found()
900 cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'],
901 required: get_option('cocoa'))
903 vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet'))
904 if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h',
905 'VMNET_BRIDGED_MODE',
908 if get_option('vmnet').enabled()
909 error('vmnet.framework API is outdated')
911 warning('vmnet.framework API is outdated, disabling')
916 seccomp_has_sysrawrc = false
917 if not get_option('seccomp').auto() or have_system or have_tools
918 seccomp = dependency('libseccomp', version: '>=2.3.0',
919 required: get_option('seccomp'),
920 method: 'pkg-config')
922 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h',
923 'SCMP_FLTATR_API_SYSRAWRC',
924 dependencies: seccomp)
928 libcap_ng = not_found
929 if not get_option('cap_ng').auto() or have_system or have_tools
930 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'],
931 required: get_option('cap_ng'))
933 if libcap_ng.found() and not cc.links('''
937 capng_capability_to_name(CAPNG_EFFECTIVE);
939 }''', dependencies: libcap_ng)
940 libcap_ng = not_found
941 if get_option('cap_ng').enabled()
942 error('could not link libcap-ng')
944 warning('could not link libcap-ng, disabling')
948 if get_option('xkbcommon').auto() and not have_system and not have_tools
949 xkbcommon = not_found
951 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'),
952 method: 'pkg-config')
956 if not get_option('slirp').auto() or have_system
957 slirp = dependency('slirp', required: get_option('slirp'),
958 method: 'pkg-config')
959 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because
960 # it passes function pointers within libslirp as callbacks for timers.
961 # When using a system-wide shared libslirp, the type information for the
962 # callback is missing and the timer call produces a false positive with CFI.
963 # Do not use the "version" keyword argument to produce a better error.
964 # with control-flow integrity.
965 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7')
966 if get_option('slirp').enabled()
967 error('Control-Flow Integrity requires libslirp 4.7.')
969 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.')
976 if not get_option('vde').auto() or have_system or have_tools
977 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'],
978 required: get_option('vde'))
980 if vde.found() and not cc.links('''
981 #include <libvdeplug.h>
984 struct vde_open_args a = {0, 0, 0};
988 }''', dependencies: vde)
990 if get_option('cap_ng').enabled()
991 error('could not link libvdeplug')
993 warning('could not link libvdeplug, disabling')
998 if not get_option('pa').auto() or (targetos == 'linux' and have_system)
999 pulse = dependency('libpulse', required: get_option('pa'),
1000 method: 'pkg-config')
1003 if not get_option('alsa').auto() or (targetos == 'linux' and have_system)
1004 alsa = dependency('alsa', required: get_option('alsa'),
1005 method: 'pkg-config')
1008 if not get_option('jack').auto() or have_system
1009 jack = dependency('jack', required: get_option('jack'),
1010 method: 'pkg-config')
1012 pipewire = not_found
1013 if not get_option('pipewire').auto() or (targetos == 'linux' and have_system)
1014 pipewire = dependency('libpipewire-0.3', version: '>=0.3.60',
1015 required: get_option('pipewire'),
1016 method: 'pkg-config')
1019 if not get_option('sndio').auto() or have_system
1020 sndio = dependency('sndio', required: get_option('sndio'),
1021 method: 'pkg-config')
1024 spice_protocol = not_found
1025 if not get_option('spice_protocol').auto() or have_system
1026 spice_protocol = dependency('spice-protocol', version: '>=0.14.0',
1027 required: get_option('spice_protocol'),
1028 method: 'pkg-config')
1031 if not get_option('spice').auto() or have_system
1032 spice = dependency('spice-server', version: '>=0.14.0',
1033 required: get_option('spice'),
1034 method: 'pkg-config')
1036 spice_headers = spice.partial_dependency(compile_args: true, includes: true)
1038 rt = cc.find_library('rt', required: false)
1040 libiscsi = not_found
1041 if not get_option('libiscsi').auto() or have_block
1042 libiscsi = dependency('libiscsi', version: '>=1.9.0',
1043 required: get_option('libiscsi'),
1044 method: 'pkg-config')
1047 if not get_option('zstd').auto() or have_block
1048 zstd = dependency('libzstd', version: '>=1.4.0',
1049 required: get_option('zstd'),
1050 method: 'pkg-config')
1054 have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found()
1055 if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu
1056 virgl = dependency('virglrenderer',
1057 method: 'pkg-config',
1058 required: get_option('virglrenderer'))
1060 config_host_data.set('HAVE_VIRGL_D3D_INFO_EXT',
1061 cc.has_member('struct virgl_renderer_resource_info_ext', 'd3d_tex2d',
1062 prefix: '#include <virglrenderer.h>',
1063 dependencies: virgl))
1067 if not get_option('blkio').auto() or have_block
1068 blkio = dependency('blkio',
1069 method: 'pkg-config',
1070 required: get_option('blkio'))
1073 if not get_option('curl').auto() or have_block
1074 curl = dependency('libcurl', version: '>=7.29.0',
1075 method: 'pkg-config',
1076 required: get_option('curl'))
1079 if targetos == 'linux' and (have_system or have_tools)
1080 libudev = dependency('libudev',
1081 method: 'pkg-config',
1082 required: get_option('libudev'))
1085 mpathlibs = [libudev]
1086 mpathpersist = not_found
1087 if targetos == 'linux' and have_tools and get_option('mpath').allowed()
1088 mpath_test_source = '''
1089 #include <libudev.h>
1090 #include <mpath_persist.h>
1091 unsigned mpath_mx_alloc_len = 1024;
1093 static struct config *multipath_conf;
1094 extern struct udev *udev;
1095 extern struct config *get_multipath_config(void);
1096 extern void put_multipath_config(struct config *conf);
1098 struct config *get_multipath_config(void) { return multipath_conf; }
1099 void put_multipath_config(struct config *conf) { }
1102 multipath_conf = mpath_lib_init();
1105 libmpathpersist = cc.find_library('mpathpersist',
1106 required: get_option('mpath'))
1107 if libmpathpersist.found()
1108 mpathlibs += libmpathpersist
1109 if get_option('prefer_static')
1110 mpathlibs += cc.find_library('devmapper',
1111 required: get_option('mpath'))
1113 mpathlibs += cc.find_library('multipath',
1114 required: get_option('mpath'))
1115 foreach lib: mpathlibs
1121 if mpathlibs.length() == 0
1122 msg = 'Dependencies missing for libmpathpersist'
1123 elif cc.links(mpath_test_source, dependencies: mpathlibs)
1124 mpathpersist = declare_dependency(dependencies: mpathlibs)
1126 msg = 'Cannot detect libmpathpersist API'
1128 if not mpathpersist.found()
1129 if get_option('mpath').enabled()
1132 warning(msg + ', disabling')
1140 if have_system and get_option('curses').allowed()
1142 #if defined(__APPLE__) || defined(__OpenBSD__)
1143 #define _XOPEN_SOURCE_EXTENDED 1
1150 setlocale(LC_ALL, "");
1152 addwstr(L"wide chars\n");
1154 add_wch(WACS_DEGREE);
1158 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw']
1159 curses = dependency(curses_dep_list,
1161 method: 'pkg-config')
1162 msg = get_option('curses').enabled() ? 'curses library not found' : ''
1163 curses_compile_args = ['-DNCURSES_WIDECHAR=1']
1165 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses])
1166 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses],
1167 version: curses.version())
1169 msg = 'curses package not usable'
1173 if not curses.found()
1174 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
1175 if targetos != 'windows' and not has_curses_h
1176 message('Trying with /usr/include/ncursesw')
1177 curses_compile_args += ['-I/usr/include/ncursesw']
1178 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
1181 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw'])
1182 foreach curses_libname : curses_libname_list
1183 libcurses = cc.find_library(curses_libname,
1185 if libcurses.found()
1186 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses)
1187 curses = declare_dependency(compile_args: curses_compile_args,
1188 dependencies: [libcurses])
1191 msg = 'curses library not usable'
1197 if get_option('iconv').allowed()
1198 foreach link_args : [ ['-liconv'], [] ]
1199 # Programs will be linked with glib and this will bring in libiconv on FreeBSD.
1200 # We need to use libiconv if available because mixing libiconv's headers with
1201 # the system libc does not work.
1202 # However, without adding glib to the dependencies -L/usr/local/lib will not be
1203 # included in the command line and libiconv will not be found.
1207 iconv_t conv = iconv_open("WCHAR_T", "UCS-2");
1208 return conv != (iconv_t) -1;
1209 }''', args: link_args, dependencies: glib)
1210 iconv = declare_dependency(link_args: link_args, dependencies: glib)
1215 if curses.found() and not iconv.found()
1216 if get_option('iconv').enabled()
1217 error('iconv not available')
1219 msg = 'iconv required for curses UI but not available'
1222 if not curses.found() and msg != ''
1223 if get_option('curses').enabled()
1226 warning(msg + ', disabling')
1232 if not get_option('brlapi').auto() or have_system
1233 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'],
1234 required: get_option('brlapi'))
1235 if brlapi.found() and not cc.links('''
1238 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi)
1240 if get_option('brlapi').enabled()
1241 error('could not link brlapi')
1243 warning('could not link brlapi, disabling')
1249 if not get_option('sdl').auto() or have_system
1250 sdl = dependency('sdl2', required: get_option('sdl'))
1251 sdl_image = not_found
1254 # Some versions of SDL have problems with -Wundef
1255 if not cc.compiles('''
1257 #include <SDL_syswm.h>
1258 int main(int argc, char *argv[]) { return 0; }
1259 ''', dependencies: sdl, args: '-Werror=undef')
1260 sdl = declare_dependency(compile_args: '-Wno-undef',
1262 version: sdl.version())
1264 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'),
1265 method: 'pkg-config')
1267 if get_option('sdl_image').enabled()
1268 error('sdl-image required, but SDL was @0@'.format(
1269 get_option('sdl').disabled() ? 'disabled' : 'not found'))
1271 sdl_image = not_found
1275 if not get_option('rbd').auto() or have_block
1276 librados = cc.find_library('rados', required: get_option('rbd'))
1277 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'],
1278 required: get_option('rbd'))
1279 if librados.found() and librbd.found()
1282 #include <rbd/librbd.h>
1285 rados_create(&cluster, NULL);
1286 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0)
1290 }''', dependencies: [librbd, librados])
1291 rbd = declare_dependency(dependencies: [librbd, librados])
1292 elif get_option('rbd').enabled()
1293 error('librbd >= 1.12.0 required')
1295 warning('librbd >= 1.12.0 not found, disabling')
1300 glusterfs = not_found
1301 glusterfs_ftruncate_has_stat = false
1302 glusterfs_iocb_has_stat = false
1303 if not get_option('glusterfs').auto() or have_block
1304 glusterfs = dependency('glusterfs-api', version: '>=3',
1305 required: get_option('glusterfs'),
1306 method: 'pkg-config')
1307 if glusterfs.found()
1308 glusterfs_ftruncate_has_stat = cc.links('''
1309 #include <glusterfs/api/glfs.h>
1314 /* new glfs_ftruncate() passes two additional args */
1315 return glfs_ftruncate(NULL, 0, NULL, NULL);
1317 ''', dependencies: glusterfs)
1318 glusterfs_iocb_has_stat = cc.links('''
1319 #include <glusterfs/api/glfs.h>
1321 /* new glfs_io_cbk() passes two additional glfs_stat structs */
1323 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
1329 glfs_io_cbk iocb = &glusterfs_iocb;
1330 iocb(NULL, 0 , NULL, NULL, NULL);
1333 ''', dependencies: glusterfs)
1338 if not get_option('libssh').auto() or have_block
1339 libssh = dependency('libssh', version: '>=0.8.7',
1340 method: 'pkg-config',
1341 required: get_option('libssh'))
1344 libbzip2 = not_found
1345 if not get_option('bzip2').auto() or have_block
1346 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'],
1347 required: get_option('bzip2'))
1348 if libbzip2.found() and not cc.links('''
1350 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2)
1351 libbzip2 = not_found
1352 if get_option('bzip2').enabled()
1353 error('could not link libbzip2')
1355 warning('could not link libbzip2, disabling')
1360 liblzfse = not_found
1361 if not get_option('lzfse').auto() or have_block
1362 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'],
1363 required: get_option('lzfse'))
1365 if liblzfse.found() and not cc.links('''
1367 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse)
1368 liblzfse = not_found
1369 if get_option('lzfse').enabled()
1370 error('could not link liblzfse')
1372 warning('could not link liblzfse, disabling')
1377 if get_option('oss').allowed() and have_system
1378 if not cc.has_header('sys/soundcard.h')
1380 elif targetos == 'netbsd'
1381 oss = cc.find_library('ossaudio', required: get_option('oss'))
1383 oss = declare_dependency()
1387 if get_option('oss').enabled()
1388 error('OSS not found')
1393 if not get_option('dsound').auto() or (targetos == 'windows' and have_system)
1394 if cc.has_header('dsound.h')
1395 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid'])
1398 if not dsound.found()
1399 if get_option('dsound').enabled()
1400 error('DirectSound not found')
1405 coreaudio = not_found
1406 if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system)
1407 coreaudio = dependency('appleframeworks', modules: 'CoreAudio',
1408 required: get_option('coreaudio'))
1412 if not get_option('opengl').auto() or have_system or have_vhost_user_gpu
1413 epoxy = dependency('epoxy', method: 'pkg-config',
1414 required: get_option('opengl'))
1415 if cc.has_header('epoxy/egl.h', dependencies: epoxy)
1417 elif get_option('opengl').enabled()
1418 error('epoxy/egl.h not found')
1422 if (have_system or have_tools) and (virgl.found() or opengl.found())
1423 gbm = dependency('gbm', method: 'pkg-config', required: false)
1425 have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found()
1428 gnutls_crypto = not_found
1429 if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system)
1430 # For general TLS support our min gnutls matches
1431 # that implied by our platform support matrix
1433 # For the crypto backends, we look for a newer
1436 # Version 3.6.8 is needed to get XTS
1437 # Version 3.6.13 is needed to get PBKDF
1438 # Version 3.6.14 is needed to get HW accelerated XTS
1440 # If newer enough gnutls isn't available, we can
1441 # still use a different crypto backend to satisfy
1442 # the platform support requirements
1443 gnutls_crypto = dependency('gnutls', version: '>=3.6.14',
1444 method: 'pkg-config',
1446 if gnutls_crypto.found()
1447 gnutls = gnutls_crypto
1449 # Our min version if all we need is TLS
1450 gnutls = dependency('gnutls', version: '>=3.5.18',
1451 method: 'pkg-config',
1452 required: get_option('gnutls'))
1456 # We prefer use of gnutls for crypto, unless the options
1457 # explicitly asked for nettle or gcrypt.
1459 # If gnutls isn't available for crypto, then we'll prefer
1460 # gcrypt over nettle for performance reasons.
1466 if get_option('nettle').enabled() and get_option('gcrypt').enabled()
1467 error('Only one of gcrypt & nettle can be enabled')
1470 # Explicit nettle/gcrypt request, so ignore gnutls for crypto
1471 if get_option('nettle').enabled() or get_option('gcrypt').enabled()
1472 gnutls_crypto = not_found
1475 if not gnutls_crypto.found()
1476 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled()
1477 gcrypt = dependency('libgcrypt', version: '>=1.8',
1478 method: 'config-tool',
1479 required: get_option('gcrypt'))
1480 # Debian has removed -lgpg-error from libgcrypt-config
1481 # as it "spreads unnecessary dependencies" which in
1482 # turn breaks static builds...
1483 if gcrypt.found() and get_option('prefer_static')
1484 gcrypt = declare_dependency(dependencies:
1486 cc.find_library('gpg-error', required: true)],
1487 version: gcrypt.version())
1490 if (not get_option('nettle').auto() or have_system) and not gcrypt.found()
1491 nettle = dependency('nettle', version: '>=3.4',
1492 method: 'pkg-config',
1493 required: get_option('nettle'))
1494 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle)
1500 gmp = dependency('gmp', required: false, method: 'pkg-config')
1501 if nettle.found() and gmp.found()
1502 hogweed = dependency('hogweed', version: '>=3.4',
1503 method: 'pkg-config',
1504 required: get_option('nettle'))
1511 have_gtk_clipboard = get_option('gtk_clipboard').enabled()
1513 if not get_option('gtk').auto() or have_system
1514 gtk = dependency('gtk+-3.0', version: '>=3.22.0',
1515 method: 'pkg-config',
1516 required: get_option('gtk'))
1518 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0',
1519 method: 'pkg-config',
1521 gtk = declare_dependency(dependencies: [gtk, gtkx11],
1522 version: gtk.version())
1524 if not get_option('vte').auto() or have_system
1525 vte = dependency('vte-2.91',
1526 method: 'pkg-config',
1527 required: get_option('vte'))
1529 elif have_gtk_clipboard
1530 error('GTK clipboard requested, but GTK not found')
1536 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found())
1539 if get_option('png').allowed() and have_system
1540 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'),
1541 method: 'pkg-config')
1546 if get_option('vnc').allowed() and have_system
1547 vnc = declare_dependency() # dummy dependency
1548 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'),
1549 method: 'pkg-config')
1550 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'],
1551 required: get_option('vnc_sasl'))
1553 sasl = declare_dependency(dependencies: sasl,
1554 compile_args: '-DSTRUCT_IOVEC_DEFINED')
1559 if not get_option('auth_pam').auto() or have_system
1560 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'],
1561 required: get_option('auth_pam'))
1563 if pam.found() and not cc.links('''
1565 #include <security/pam_appl.h>
1567 const char *service_name = "qemu";
1568 const char *user = "frank";
1569 const struct pam_conv pam_conv = { 0 };
1570 pam_handle_t *pamh = NULL;
1571 pam_start(service_name, user, &pam_conv, &pamh);
1573 }''', dependencies: pam)
1575 if get_option('auth_pam').enabled()
1576 error('could not link libpam')
1578 warning('could not link libpam, disabling')
1583 if not get_option('snappy').auto() or have_system
1584 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'],
1585 required: get_option('snappy'))
1587 if snappy.found() and not cc.links('''
1588 #include <snappy-c.h>
1589 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy)
1591 if get_option('snappy').enabled()
1592 error('could not link libsnappy')
1594 warning('could not link libsnappy, disabling')
1599 if not get_option('lzo').auto() or have_system
1600 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'],
1601 required: get_option('lzo'))
1603 if lzo.found() and not cc.links('''
1604 #include <lzo/lzo1x.h>
1605 int main(void) { lzo_version(); return 0; }''', dependencies: lzo)
1607 if get_option('lzo').enabled()
1608 error('could not link liblzo2')
1610 warning('could not link liblzo2, disabling')
1615 if not get_option('numa').auto() or have_system or have_tools
1616 numa = cc.find_library('numa', has_headers: ['numa.h'],
1617 required: get_option('numa'))
1619 if numa.found() and not cc.links('''
1621 int main(void) { return numa_available(); }
1622 ''', dependencies: numa)
1624 if get_option('numa').enabled()
1625 error('could not link numa')
1627 warning('could not link numa, disabling')
1632 if not get_option('rdma').auto() or have_system
1633 libumad = cc.find_library('ibumad', required: get_option('rdma'))
1634 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'],
1635 required: get_option('rdma')),
1636 cc.find_library('ibverbs', required: get_option('rdma')),
1638 rdma = declare_dependency(dependencies: rdma_libs)
1639 foreach lib: rdma_libs
1647 if get_option('xen').enabled() or (get_option('xen').auto() and have_system)
1648 xencontrol = dependency('xencontrol', required: false,
1649 method: 'pkg-config')
1650 if xencontrol.found()
1651 xen_pc = declare_dependency(version: xencontrol.version(),
1654 # disabler: true makes xen_pc.found() return false if any is not found
1655 dependency('xenstore', required: false,
1656 method: 'pkg-config',
1658 dependency('xenforeignmemory', required: false,
1659 method: 'pkg-config',
1661 dependency('xengnttab', required: false,
1662 method: 'pkg-config',
1664 dependency('xenevtchn', required: false,
1665 method: 'pkg-config',
1667 dependency('xendevicemodel', required: false,
1668 method: 'pkg-config',
1670 # optional, no "disabler: true"
1671 dependency('xentoolcore', required: false,
1672 method: 'pkg-config')])
1678 xen_tests = [ '4.11.0', '4.10.0', '4.9.0', '4.8.0', '4.7.1' ]
1680 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1681 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1682 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1683 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1684 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1687 foreach ver: xen_tests
1688 # cache the various library tests to avoid polluting the logs
1690 foreach l: xen_libs[ver]
1691 if l not in xen_deps
1692 xen_deps += { l: cc.find_library(l, required: false) }
1694 xen_test_deps += xen_deps[l]
1697 # Use -D to pick just one of the test programs in scripts/xen-detect.c
1698 xen_version = ver.split('.')
1699 xen_ctrl_version = xen_version[0] + \
1700 ('0' + xen_version[1]).substring(-2) + \
1701 ('0' + xen_version[2]).substring(-2)
1702 if cc.links(files('scripts/xen-detect.c'),
1703 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version,
1704 dependencies: xen_test_deps)
1705 xen = declare_dependency(version: ver, dependencies: xen_test_deps)
1711 accelerators += 'CONFIG_XEN'
1712 elif get_option('xen').enabled()
1713 error('could not compile and link Xen test program')
1716 have_xen_pci_passthrough = get_option('xen_pci_passthrough') \
1717 .require(xen.found(),
1718 error_message: 'Xen PCI passthrough requested but Xen not enabled') \
1719 .require(targetos == 'linux',
1720 error_message: 'Xen PCI passthrough not available on this platform') \
1721 .require(cpu == 'x86' or cpu == 'x86_64',
1722 error_message: 'Xen PCI passthrough not available on this platform') \
1727 if not get_option('smartcard').auto() or have_system
1728 cacard = dependency('libcacard', required: get_option('smartcard'),
1729 version: '>=2.5.1', method: 'pkg-config')
1733 u2f = dependency('u2f-emu', required: get_option('u2f'),
1734 method: 'pkg-config')
1738 canokey = dependency('canokey-qemu', required: get_option('canokey'),
1739 method: 'pkg-config')
1741 usbredir = not_found
1742 if not get_option('usb_redir').auto() or have_system
1743 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'),
1744 version: '>=0.6', method: 'pkg-config')
1747 if not get_option('libusb').auto() or have_system
1748 libusb = dependency('libusb-1.0', required: get_option('libusb'),
1749 version: '>=1.0.13', method: 'pkg-config')
1753 if not get_option('libpmem').auto() or have_system
1754 libpmem = dependency('libpmem', required: get_option('libpmem'),
1755 method: 'pkg-config')
1757 libdaxctl = not_found
1758 if not get_option('libdaxctl').auto() or have_system
1759 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'),
1760 version: '>=57', method: 'pkg-config')
1764 tasn1 = dependency('libtasn1',
1765 method: 'pkg-config')
1767 keyutils = not_found
1768 if get_option('keyring').enabled()
1769 keyutils = dependency('libkeyutils', required: false, method: 'pkg-config')
1772 has_gettid = cc.has_function('gettid')
1775 selinux = dependency('libselinux',
1776 required: get_option('selinux'),
1777 method: 'pkg-config')
1782 if get_option('malloc') == 'system'
1784 get_option('malloc_trim').allowed() and \
1785 cc.has_function('malloc_trim', prefix: '#include <malloc.h>')
1787 has_malloc_trim = false
1788 malloc = cc.find_library(get_option('malloc'), required: true)
1790 if not has_malloc_trim and get_option('malloc_trim').enabled()
1791 if get_option('malloc') == 'system'
1792 error('malloc_trim not available on this platform.')
1794 error('malloc_trim not available with non-libc memory allocator')
1798 gnu_source_prefix = '''
1804 # Check whether the glibc provides STATX_BASIC_STATS
1806 has_statx = cc.has_header_symbol('sys/stat.h', 'STATX_BASIC_STATS', prefix: gnu_source_prefix)
1808 # Check whether statx() provides mount ID information
1810 has_statx_mnt_id = cc.has_header_symbol('sys/stat.h', 'STATX_MNT_ID', prefix: gnu_source_prefix)
1812 have_vhost_user_blk_server = get_option('vhost_user_blk_server') \
1813 .require(targetos == 'linux',
1814 error_message: 'vhost_user_blk_server requires linux') \
1815 .require(have_vhost_user,
1816 error_message: 'vhost_user_blk_server requires vhost-user support') \
1817 .disable_auto_if(not have_tools and not have_system) \
1820 if get_option('fuse').disabled() and get_option('fuse_lseek').enabled()
1821 error('Cannot enable fuse-lseek while fuse is disabled')
1824 fuse = dependency('fuse3', required: get_option('fuse'),
1825 version: '>=3.1', method: 'pkg-config')
1827 fuse_lseek = not_found
1828 if get_option('fuse_lseek').allowed()
1829 if fuse.version().version_compare('>=3.8')
1831 fuse_lseek = declare_dependency()
1832 elif get_option('fuse_lseek').enabled()
1834 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version())
1836 error('fuse-lseek requires libfuse, which was not found')
1841 have_libvduse = (targetos == 'linux')
1842 if get_option('libvduse').enabled()
1843 if targetos != 'linux'
1844 error('libvduse requires linux')
1846 elif get_option('libvduse').disabled()
1847 have_libvduse = false
1850 have_vduse_blk_export = (have_libvduse and targetos == 'linux')
1851 if get_option('vduse_blk_export').enabled()
1852 if targetos != 'linux'
1853 error('vduse_blk_export requires linux')
1854 elif not have_libvduse
1855 error('vduse_blk_export requires libvduse support')
1857 elif get_option('vduse_blk_export').disabled()
1858 have_vduse_blk_export = false
1862 libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config')
1863 if libbpf.found() and not cc.links('''
1864 #include <bpf/libbpf.h>
1867 bpf_object__destroy_skeleton(NULL);
1869 }''', dependencies: libbpf)
1871 if get_option('bpf').enabled()
1872 error('libbpf skeleton test failed')
1874 warning('libbpf skeleton test failed, disabling')
1880 if not get_option('libdw').auto() or \
1881 (not get_option('prefer_static') and (have_system or have_user))
1882 libdw = dependency('libdw',
1883 method: 'pkg-config',
1884 required: get_option('libdw'))
1891 audio_drivers_selected = []
1893 audio_drivers_available = {
1894 'alsa': alsa.found(),
1895 'coreaudio': coreaudio.found(),
1896 'dsound': dsound.found(),
1897 'jack': jack.found(),
1899 'pa': pulse.found(),
1900 'pipewire': pipewire.found(),
1902 'sndio': sndio.found(),
1904 foreach k, v: audio_drivers_available
1905 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v)
1908 # Default to native drivers first, OSS second, SDL third
1909 audio_drivers_priority = \
1910 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \
1911 (targetos == 'linux' ? [] : [ 'sdl' ])
1912 audio_drivers_default = []
1913 foreach k: audio_drivers_priority
1914 if audio_drivers_available[k]
1915 audio_drivers_default += k
1919 foreach k: get_option('audio_drv_list')
1921 audio_drivers_selected += audio_drivers_default
1922 elif not audio_drivers_available[k]
1923 error('Audio driver "@0@" not available.'.format(k))
1925 audio_drivers_selected += k
1929 config_host_data.set('CONFIG_AUDIO_DRIVERS',
1930 '"' + '", "'.join(audio_drivers_selected) + '", ')
1932 if get_option('cfi')
1934 # Check for dependency on LTO
1935 if not get_option('b_lto')
1936 error('Selected Control-Flow Integrity but LTO is disabled')
1939 error('Selected Control-Flow Integrity is not compatible with modules')
1941 # Check for cfi flags. CFI requires LTO so we can't use
1942 # get_supported_arguments, but need a more complex "compiles" which allows
1944 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall',
1945 args: ['-flto', '-fsanitize=cfi-icall'] )
1946 cfi_flags += '-fsanitize=cfi-icall'
1948 error('-fsanitize=cfi-icall is not supported by the compiler')
1950 if cc.compiles('int main () { return 0; }',
1951 name: '-fsanitize-cfi-icall-generalize-pointers',
1952 args: ['-flto', '-fsanitize=cfi-icall',
1953 '-fsanitize-cfi-icall-generalize-pointers'] )
1954 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers'
1956 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler')
1958 if get_option('cfi_debug')
1959 if cc.compiles('int main () { return 0; }',
1960 name: '-fno-sanitize-trap=cfi-icall',
1961 args: ['-flto', '-fsanitize=cfi-icall',
1962 '-fno-sanitize-trap=cfi-icall'] )
1963 cfi_flags += '-fno-sanitize-trap=cfi-icall'
1965 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler')
1968 add_global_arguments(cfi_flags, native: false, language: all_languages)
1969 add_global_link_arguments(cfi_flags, native: false, language: all_languages)
1972 have_host_block_device = (targetos != 'darwin' or
1973 cc.has_header('IOKit/storage/IOMedia.h'))
1975 dbus_display = get_option('dbus_display') \
1976 .require(gio.version().version_compare('>=2.64'),
1977 error_message: '-display dbus requires glib>=2.64') \
1978 .require(gdbus_codegen.found(),
1979 error_message: gdbus_codegen_error.format('-display dbus')) \
1982 have_virtfs = get_option('virtfs') \
1983 .require(targetos == 'linux' or targetos == 'darwin',
1984 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \
1985 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'),
1986 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \
1987 .require(targetos == 'darwin' or libattr.found(),
1988 error_message: 'virtio-9p (virtfs) on Linux requires libattr-devel') \
1989 .disable_auto_if(not have_tools and not have_system) \
1992 have_virtfs_proxy_helper = get_option('virtfs_proxy_helper') \
1993 .require(targetos != 'darwin', error_message: 'the virtfs proxy helper is incompatible with macOS') \
1994 .require(have_virtfs, error_message: 'the virtfs proxy helper requires that virtfs is enabled') \
1995 .disable_auto_if(not have_tools) \
1996 .require(libcap_ng.found(), error_message: 'the virtfs proxy helper requires libcap-ng') \
1999 if get_option('block_drv_ro_whitelist') == ''
2000 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '')
2002 config_host_data.set('CONFIG_BDRV_RO_WHITELIST',
2003 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ')
2005 if get_option('block_drv_rw_whitelist') == ''
2006 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '')
2008 config_host_data.set('CONFIG_BDRV_RW_WHITELIST',
2009 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ')
2012 foreach k : get_option('trace_backends')
2013 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true)
2015 config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file'))
2016 config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority'))
2018 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path())
2020 config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir'))
2021 config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix'))
2022 config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir)
2023 config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir)
2024 config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir)
2026 qemu_firmwarepath = ''
2027 foreach k : get_option('qemu_firmwarepath')
2028 qemu_firmwarepath += '"' + get_option('prefix') / k + '", '
2030 config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath)
2032 config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir'))
2033 config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir)
2034 config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir'))
2035 config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir'))
2036 config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir)
2037 config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir'))
2040 config_host_data.set('CONFIG_STAMP', run_command(
2041 meson.current_source_dir() / 'scripts/qemu-stamp.py',
2042 meson.project_version(), get_option('pkgversion'), '--',
2043 meson.current_source_dir() / 'configure',
2044 capture: true, check: true).stdout().strip())
2047 have_slirp_smbd = get_option('slirp_smbd') \
2048 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \
2051 smbd_path = get_option('smbd')
2053 smbd_path = (targetos == 'solaris' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd')
2055 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path)
2058 config_host_data.set('HOST_' + host_arch.to_upper(), 1)
2060 if get_option('module_upgrades') and not enable_modules
2061 error('Cannot enable module-upgrades as modules are not enabled')
2063 config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades'))
2065 config_host_data.set('CONFIG_ATTR', libattr.found())
2066 config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools'))
2067 config_host_data.set('CONFIG_BRLAPI', brlapi.found())
2068 config_host_data.set('CONFIG_COCOA', cocoa.found())
2069 config_host_data.set('CONFIG_FUZZ', get_option('fuzzing'))
2070 config_host_data.set('CONFIG_GCOV', get_option('b_coverage'))
2071 config_host_data.set('CONFIG_LIBUDEV', libudev.found())
2072 config_host_data.set('CONFIG_LZO', lzo.found())
2073 config_host_data.set('CONFIG_MPATH', mpathpersist.found())
2074 config_host_data.set('CONFIG_BLKIO', blkio.found())
2076 config_host_data.set('CONFIG_BLKIO_VHOST_VDPA_FD',
2077 blkio.version().version_compare('>=1.3.0'))
2079 config_host_data.set('CONFIG_CURL', curl.found())
2080 config_host_data.set('CONFIG_CURSES', curses.found())
2081 config_host_data.set('CONFIG_GBM', gbm.found())
2082 config_host_data.set('CONFIG_GIO', gio.found())
2083 config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found())
2084 if glusterfs.found()
2085 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4'))
2086 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5'))
2087 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6'))
2088 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6'))
2089 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat)
2090 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat)
2092 config_host_data.set('CONFIG_GTK', gtk.found())
2093 config_host_data.set('CONFIG_VTE', vte.found())
2094 config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard)
2095 config_host_data.set('CONFIG_HEXAGON_IDEF_PARSER', get_option('hexagon_idef_parser'))
2096 config_host_data.set('CONFIG_LIBATTR', have_old_libattr)
2097 config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found())
2098 config_host_data.set('CONFIG_EBPF', libbpf.found())
2099 config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found())
2100 config_host_data.set('CONFIG_LIBISCSI', libiscsi.found())
2101 config_host_data.set('CONFIG_LIBNFS', libnfs.found())
2102 config_host_data.set('CONFIG_LIBSSH', libssh.found())
2103 config_host_data.set('CONFIG_LINUX_AIO', libaio.found())
2104 config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found())
2105 config_host_data.set('CONFIG_LIBPMEM', libpmem.found())
2106 config_host_data.set('CONFIG_MODULES', enable_modules)
2107 config_host_data.set('CONFIG_NUMA', numa.found())
2109 config_host_data.set('HAVE_NUMA_HAS_PREFERRED_MANY',
2110 cc.has_function('numa_has_preferred_many',
2111 dependencies: numa))
2113 config_host_data.set('CONFIG_OPENGL', opengl.found())
2114 config_host_data.set('CONFIG_RBD', rbd.found())
2115 config_host_data.set('CONFIG_RDMA', rdma.found())
2116 config_host_data.set('CONFIG_SAFESTACK', get_option('safe_stack'))
2117 config_host_data.set('CONFIG_SDL', sdl.found())
2118 config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found())
2119 config_host_data.set('CONFIG_SECCOMP', seccomp.found())
2121 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc)
2123 config_host_data.set('CONFIG_SNAPPY', snappy.found())
2124 config_host_data.set('CONFIG_TPM', have_tpm)
2125 config_host_data.set('CONFIG_TSAN', get_option('tsan'))
2126 config_host_data.set('CONFIG_USB_LIBUSB', libusb.found())
2127 config_host_data.set('CONFIG_VDE', vde.found())
2128 config_host_data.set('CONFIG_VHOST_NET', have_vhost_net)
2129 config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user)
2130 config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa)
2131 config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel)
2132 config_host_data.set('CONFIG_VHOST_USER', have_vhost_user)
2133 config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto)
2134 config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa)
2135 config_host_data.set('CONFIG_VMNET', vmnet.found())
2136 config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server)
2137 config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export)
2138 config_host_data.set('CONFIG_PNG', png.found())
2139 config_host_data.set('CONFIG_VNC', vnc.found())
2140 config_host_data.set('CONFIG_VNC_JPEG', jpeg.found())
2141 config_host_data.set('CONFIG_VNC_SASL', sasl.found())
2142 config_host_data.set('CONFIG_VIRTFS', have_virtfs)
2143 config_host_data.set('CONFIG_VTE', vte.found())
2144 config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found())
2145 config_host_data.set('CONFIG_KEYUTILS', keyutils.found())
2146 config_host_data.set('CONFIG_GETTID', has_gettid)
2147 config_host_data.set('CONFIG_GNUTLS', gnutls.found())
2148 config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found())
2149 config_host_data.set('CONFIG_TASN1', tasn1.found())
2150 config_host_data.set('CONFIG_GCRYPT', gcrypt.found())
2151 config_host_data.set('CONFIG_NETTLE', nettle.found())
2152 config_host_data.set('CONFIG_HOGWEED', hogweed.found())
2153 config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private')
2154 config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim)
2155 config_host_data.set('CONFIG_STATX', has_statx)
2156 config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id)
2157 config_host_data.set('CONFIG_ZSTD', zstd.found())
2158 config_host_data.set('CONFIG_FUSE', fuse.found())
2159 config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found())
2160 config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found())
2161 if spice_protocol.found()
2162 config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0])
2163 config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1])
2164 config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2])
2166 config_host_data.set('CONFIG_SPICE', spice.found())
2167 config_host_data.set('CONFIG_X11', x11.found())
2168 config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display)
2169 config_host_data.set('CONFIG_CFI', get_option('cfi'))
2170 config_host_data.set('CONFIG_SELINUX', selinux.found())
2171 config_host_data.set('CONFIG_XEN_BACKEND', xen.found())
2172 config_host_data.set('CONFIG_LIBDW', libdw.found())
2174 # protect from xen.version() having less than three components
2175 xen_version = xen.version().split('.') + ['0', '0']
2176 xen_ctrl_version = xen_version[0] + \
2177 ('0' + xen_version[1]).substring(-2) + \
2178 ('0' + xen_version[2]).substring(-2)
2179 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version)
2181 config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version()))
2182 config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0])
2183 config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1])
2184 config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2])
2186 config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf)
2187 config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device)
2189 have_coroutine_pool = get_option('coroutine_pool')
2190 if get_option('debug_stack_usage') and have_coroutine_pool
2191 message('Disabling coroutine pool to measure stack usage')
2192 have_coroutine_pool = false
2194 config_host_data.set10('CONFIG_COROUTINE_POOL', have_coroutine_pool)
2195 config_host_data.set('CONFIG_DEBUG_GRAPH_LOCK', get_option('debug_graph_lock'))
2196 config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex'))
2197 config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage'))
2198 config_host_data.set('CONFIG_GPROF', get_option('gprof'))
2199 config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed())
2200 config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug'))
2201 config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed())
2204 config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h'))
2205 config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h'))
2206 config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h'))
2207 config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h'))
2208 config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h'))
2209 config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h'))
2210 config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h'))
2211 config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h'))
2212 config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h'))
2213 if targetos == 'windows'
2214 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h'))
2218 config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range'))
2219 config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4'))
2220 config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime'))
2221 config_host_data.set('CONFIG_DUP3', cc.has_function('dup3'))
2222 config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate'))
2223 config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate'))
2224 config_host_data.set('CONFIG_GETCPU', cc.has_function('getcpu', prefix: gnu_source_prefix))
2225 config_host_data.set('CONFIG_SCHED_GETCPU', cc.has_function('sched_getcpu', prefix: '#include <sched.h>'))
2226 # Note that we need to specify prefix: here to avoid incorrectly
2227 # thinking that Windows has posix_memalign()
2228 config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>'))
2229 config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc'))
2230 config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc'))
2231 config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign'))
2232 config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll'))
2233 config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>'))
2234 config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np'))
2235 config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile'))
2236 config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare'))
2237 config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs'))
2238 config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range'))
2239 config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create'))
2240 config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range'))
2241 config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs'))
2242 config_host_data.set('HAVE_GLIB_WITH_SLICE_ALLOCATOR', glib_has_gslice)
2243 config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util))
2244 config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul'))
2245 config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>'))
2247 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS',
2248 cc.has_function('rbd_namespace_exists',
2250 prefix: '#include <rbd/librbd.h>'))
2253 config_host_data.set('HAVE_IBV_ADVISE_MR',
2254 cc.has_function('ibv_advise_mr',
2256 prefix: '#include <infiniband/verbs.h>'))
2259 have_asan_fiber = false
2260 if get_option('sanitizers') and \
2261 not cc.has_function('__sanitizer_start_switch_fiber',
2262 args: '-fsanitize=address',
2263 prefix: '#include <sanitizer/asan_interface.h>')
2264 warning('Missing ASAN due to missing fiber annotation interface')
2265 warning('Without code annotation, the report may be inferior.')
2267 have_asan_fiber = true
2269 config_host_data.set('CONFIG_ASAN_IFACE_FIBER', have_asan_fiber)
2272 config_host_data.set('CONFIG_BLKZONED',
2273 cc.has_header_symbol('linux/blkzoned.h', 'BLKOPENZONE'))
2274 config_host_data.set('CONFIG_EPOLL_CREATE1',
2275 cc.has_header_symbol('sys/epoll.h', 'epoll_create1'))
2276 config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE',
2277 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and
2278 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE'))
2279 config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE',
2280 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE'))
2281 config_host_data.set('CONFIG_FIEMAP',
2282 cc.has_header('linux/fiemap.h') and
2283 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP'))
2284 config_host_data.set('CONFIG_GETRANDOM',
2285 cc.has_function('getrandom') and
2286 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK'))
2287 config_host_data.set('CONFIG_INOTIFY',
2288 cc.has_header_symbol('sys/inotify.h', 'inotify_init'))
2289 config_host_data.set('CONFIG_INOTIFY1',
2290 cc.has_header_symbol('sys/inotify.h', 'inotify_init1'))
2291 config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK',
2292 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK'))
2293 config_host_data.set('CONFIG_RTNETLINK',
2294 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN'))
2295 config_host_data.set('CONFIG_SYSMACROS',
2296 cc.has_header_symbol('sys/sysmacros.h', 'makedev'))
2297 config_host_data.set('HAVE_OPTRESET',
2298 cc.has_header_symbol('getopt.h', 'optreset'))
2299 config_host_data.set('HAVE_IPPROTO_MPTCP',
2300 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP'))
2303 config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID',
2304 cc.has_member('struct sigevent', 'sigev_notify_thread_id',
2305 prefix: '#include <signal.h>'))
2306 config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM',
2307 cc.has_member('struct stat', 'st_atim',
2308 prefix: '#include <sys/stat.h>'))
2309 config_host_data.set('HAVE_BLK_ZONE_REP_CAPACITY',
2310 cc.has_member('struct blk_zone', 'capacity',
2311 prefix: '#include <linux/blkzoned.h>'))
2314 config_host_data.set('CONFIG_IOVEC',
2315 cc.has_type('struct iovec',
2316 prefix: '#include <sys/uio.h>'))
2317 config_host_data.set('HAVE_UTMPX',
2318 cc.has_type('struct utmpx',
2319 prefix: '#include <utmpx.h>'))
2321 config_host_data.set('CONFIG_EVENTFD', cc.links('''
2322 #include <sys/eventfd.h>
2323 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }'''))
2324 config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + '''
2327 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
2328 return fdatasync(0);
2330 #error Not supported
2334 has_madvise = cc.links(gnu_source_prefix + '''
2335 #include <sys/types.h>
2336 #include <sys/mman.h>
2338 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''')
2339 missing_madvise_proto = false
2341 # Some platforms (illumos and Solaris before Solaris 11) provide madvise()
2342 # but forget to prototype it. In this case, has_madvise will be true (the
2343 # test program links despite a compile warning). To detect the
2344 # missing-prototype case, we try again with a definitely-bogus prototype.
2345 # This will only compile if the system headers don't provide the prototype;
2346 # otherwise the conflicting prototypes will cause a compiler error.
2347 missing_madvise_proto = cc.links(gnu_source_prefix + '''
2348 #include <sys/types.h>
2349 #include <sys/mman.h>
2351 extern int madvise(int);
2352 int main(void) { return madvise(0); }''')
2354 config_host_data.set('CONFIG_MADVISE', has_madvise)
2355 config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto)
2357 config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + '''
2358 #include <sys/mman.h>
2359 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }'''))
2360 config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + '''
2362 #if !defined(AT_EMPTY_PATH)
2363 # error missing definition
2365 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
2367 config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + '''
2368 #include <sys/mman.h>
2370 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }'''))
2372 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + '''
2373 #include <pthread.h>
2375 static void *f(void *p) { return NULL; }
2379 pthread_create(&thread, 0, f, 0);
2380 pthread_setname_np(thread, "QEMU");
2382 }''', dependencies: threads))
2383 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + '''
2384 #include <pthread.h>
2386 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
2390 pthread_create(&thread, 0, f, 0);
2392 }''', dependencies: threads))
2393 config_host_data.set('CONFIG_PTHREAD_SET_NAME_NP', cc.links(gnu_source_prefix + '''
2394 #include <pthread.h>
2395 #include <pthread_np.h>
2397 static void *f(void *p) { return NULL; }
2401 pthread_create(&thread, 0, f, 0);
2402 pthread_set_name_np(thread, "QEMU");
2404 }''', dependencies: threads))
2405 config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + '''
2406 #include <pthread.h>
2411 pthread_condattr_t attr
2412 pthread_condattr_init(&attr);
2413 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC);
2415 }''', dependencies: threads))
2416 config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + '''
2417 #include <pthread.h>
2419 static void *f(void *p) { return NULL; }
2422 int setsize = CPU_ALLOC_SIZE(64);
2425 pthread_create(&thread, 0, f, 0);
2426 cpuset = CPU_ALLOC(64);
2427 CPU_ZERO_S(setsize, cpuset);
2428 pthread_setaffinity_np(thread, setsize, cpuset);
2429 pthread_getaffinity_np(thread, setsize, cpuset);
2432 }''', dependencies: threads))
2433 config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + '''
2434 #include <sys/signalfd.h>
2436 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }'''))
2437 config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + '''
2445 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
2446 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
2450 config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + '''
2451 #include <sys/mman.h>
2453 return mlockall(MCL_FUTURE);
2457 if get_option('l2tpv3').allowed() and have_system
2458 have_l2tpv3 = cc.has_type('struct mmsghdr',
2459 prefix: gnu_source_prefix + '''
2460 #include <sys/socket.h>
2461 #include <linux/ip.h>''')
2463 config_host_data.set('CONFIG_L2TPV3', have_l2tpv3)
2466 if get_option('netmap').allowed() and have_system
2467 have_netmap = cc.compiles('''
2468 #include <inttypes.h>
2470 #include <net/netmap.h>
2471 #include <net/netmap_user.h>
2472 #if (NETMAP_API < 11) || (NETMAP_API > 15)
2475 int main(void) { return 0; }''')
2476 if not have_netmap and get_option('netmap').enabled()
2477 error('Netmap headers not available')
2480 config_host_data.set('CONFIG_NETMAP', have_netmap)
2482 # Work around a system header bug with some kernel/XFS header
2483 # versions where they both try to define 'struct fsxattr':
2484 # xfs headers will not try to redefine structs from linux headers
2485 # if this macro is set.
2486 config_host_data.set('HAVE_FSXATTR', cc.links('''
2487 #include <linux/fs.h>
2493 # Some versions of Mac OS X incorrectly define SIZE_MAX
2494 config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles('''
2498 return printf("%zu", SIZE_MAX);
2499 }''', args: ['-Werror']))
2501 # See if 64-bit atomic operations are supported.
2502 # Note that without __atomic builtins, we can only
2503 # assume atomic loads/stores max at pointer size.
2504 config_host_data.set('CONFIG_ATOMIC64', cc.links('''
2508 uint64_t x = 0, y = 0;
2509 y = __atomic_load_n(&x, __ATOMIC_RELAXED);
2510 __atomic_store_n(&x, y, __ATOMIC_RELAXED);
2511 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2512 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
2513 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
2517 has_int128_type = cc.compiles('''
2520 int main(void) { b = a; }''')
2521 config_host_data.set('CONFIG_INT128_TYPE', has_int128_type)
2523 has_int128 = has_int128_type and cc.links('''
2532 config_host_data.set('CONFIG_INT128', has_int128)
2535 # "do we have 128-bit atomics which are handled inline and specifically not
2536 # via libatomic". The reason we can't use libatomic is documented in the
2537 # comment starting "GCC is a house divided" in include/qemu/atomic128.h.
2538 # We only care about these operations on 16-byte aligned pointers, so
2539 # force 16-byte alignment of the pointer, which may be greater than
2540 # __alignof(unsigned __int128) for the host.
2541 atomic_test_128 = '''
2542 int main(int ac, char **av) {
2543 __uint128_t *p = __builtin_assume_aligned(av[ac - 1], 16);
2544 p[1] = __atomic_load_n(&p[0], __ATOMIC_RELAXED);
2545 __atomic_store_n(&p[2], p[3], __ATOMIC_RELAXED);
2546 __atomic_compare_exchange_n(&p[4], &p[5], p[6], 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2549 has_atomic128 = cc.links(atomic_test_128)
2551 config_host_data.set('CONFIG_ATOMIC128', has_atomic128)
2553 if not has_atomic128
2554 # Even with __builtin_assume_aligned, the above test may have failed
2555 # without optimization enabled. Try again with optimizations locally
2556 # enabled for the function. See
2557 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=107389
2558 has_atomic128_opt = cc.links('__attribute__((optimize("O1")))' + atomic_test_128)
2559 config_host_data.set('CONFIG_ATOMIC128_OPT', has_atomic128_opt)
2561 if not has_atomic128_opt
2562 config_host_data.set('CONFIG_CMPXCHG128', cc.links('''
2565 __uint128_t x = 0, y = 0;
2566 __sync_val_compare_and_swap_16(&x, y, x);
2574 config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + '''
2575 #include <sys/auxv.h>
2577 return getauxval(AT_HWCAP) == 0;
2580 config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles('''
2581 #include <linux/usbdevice_fs.h>
2583 #ifndef USBDEVFS_GET_CAPABILITIES
2584 #error "USBDEVFS_GET_CAPABILITIES undefined"
2587 #ifndef USBDEVFS_DISCONNECT_CLAIM
2588 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
2591 int main(void) { return 0; }'''))
2593 have_keyring = get_option('keyring') \
2594 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \
2595 .require(cc.compiles('''
2597 #include <asm/unistd.h>
2598 #include <linux/keyctl.h>
2599 #include <sys/syscall.h>
2602 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
2603 }'''), error_message: 'keyctl syscall not available on this system').allowed()
2604 config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring)
2606 have_cpuid_h = cc.links('''
2609 unsigned a, b, c, d;
2610 unsigned max = __get_cpuid_max(0, 0);
2613 __cpuid(1, a, b, c, d);
2617 __cpuid_count(7, 0, a, b, c, d);
2622 config_host_data.set('CONFIG_CPUID_H', have_cpuid_h)
2624 config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \
2625 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \
2626 .require(cc.links('''
2628 #include <immintrin.h>
2629 static int __attribute__((target("avx2"))) bar(void *a) {
2630 __m256i x = *(__m256i *)a;
2631 return _mm256_testz_si256(x, x);
2633 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2634 '''), error_message: 'AVX2 not available').allowed())
2636 config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \
2637 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \
2638 .require(cc.links('''
2640 #include <immintrin.h>
2641 static int __attribute__((target("avx512f"))) bar(void *a) {
2642 __m512i x = *(__m512i *)a;
2643 return _mm512_test_epi64_mask(x, x);
2645 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2646 '''), error_message: 'AVX512F not available').allowed())
2648 config_host_data.set('CONFIG_AVX512BW_OPT', get_option('avx512bw') \
2649 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512BW') \
2650 .require(cc.links('''
2652 #include <immintrin.h>
2653 static int __attribute__((target("avx512bw"))) bar(void *a) {
2655 __m512i res= _mm512_abs_epi8(*x);
2658 int main(int argc, char *argv[]) { return bar(argv[0]); }
2659 '''), error_message: 'AVX512BW not available').allowed())
2661 # For both AArch64 and AArch32, detect if builtins are available.
2662 config_host_data.set('CONFIG_ARM_AES_BUILTIN', cc.compiles('''
2663 #include <arm_neon.h>
2664 #ifndef __ARM_FEATURE_AES
2665 __attribute__((target("+crypto")))
2667 void foo(uint8x16_t *p) { *p = vaesmcq_u8(*p); }
2670 have_pvrdma = get_option('pvrdma') \
2671 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \
2672 .require(cc.compiles(gnu_source_prefix + '''
2673 #include <sys/mman.h>
2678 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
2681 }'''), error_message: 'PVRDMA requires mremap').allowed()
2684 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links('''
2685 #include <infiniband/verbs.h>
2689 struct ibv_pd *pd = NULL;
2695 mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
2701 if get_option('membarrier').disabled()
2702 have_membarrier = false
2703 elif targetos == 'windows'
2704 have_membarrier = true
2705 elif targetos == 'linux'
2706 have_membarrier = cc.compiles('''
2707 #include <linux/membarrier.h>
2708 #include <sys/syscall.h>
2712 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
2713 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
2717 config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \
2718 .require(have_membarrier, error_message: 'membarrier system call not available') \
2721 have_afalg = get_option('crypto_afalg') \
2722 .require(cc.compiles(gnu_source_prefix + '''
2724 #include <sys/types.h>
2725 #include <sys/socket.h>
2726 #include <linux/if_alg.h>
2729 sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
2732 '''), error_message: 'AF_ALG requested but could not be detected').allowed()
2733 config_host_data.set('CONFIG_AF_ALG', have_afalg)
2735 config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol(
2736 'linux/vm_sockets.h', 'AF_VSOCK',
2737 prefix: '#include <sys/socket.h>',
2741 have_vss_sdk = false # old xp/2003 SDK
2742 if targetos == 'windows' and 'cpp' in all_languages
2743 have_vss = cxx.compiles('''
2744 #define __MIDL_user_allocate_free_DEFINED__
2746 int main(void) { return VSS_CTX_BACKUP; }''')
2747 have_vss_sdk = cxx.has_header('vscoordint.h')
2749 config_host_data.set('HAVE_VSS_SDK', have_vss_sdk)
2751 foreach k, v: config_host
2752 if k.startswith('CONFIG_')
2753 config_host_data.set(k, v == 'y' ? 1 : v)
2757 # Older versions of MinGW do not import _lock_file and _unlock_file properly.
2758 # This was fixed for v6.0.0 with commit b48e3ac8969d.
2759 if targetos == 'windows'
2760 config_host_data.set('HAVE__LOCK_FILE', cc.links('''
2766 }''', name: '_lock_file and _unlock_file'))
2769 if targetos == 'windows'
2770 mingw_has_setjmp_longjmp = cc.links('''
2774 * These functions are not available in setjmp header, but may be
2775 * available at link time, from libmingwex.a.
2777 extern int __mingw_setjmp(jmp_buf);
2778 extern void __attribute__((noreturn)) __mingw_longjmp(jmp_buf, int);
2780 __mingw_setjmp(env);
2781 __mingw_longjmp(env, 0);
2783 ''', name: 'mingw setjmp and longjmp')
2785 if cpu == 'aarch64' and not mingw_has_setjmp_longjmp
2786 error('mingw must provide setjmp/longjmp for windows-arm64')
2790 ########################
2791 # Target configuration #
2792 ########################
2794 minikconf = find_program('scripts/minikconf.py')
2796 config_all_devices = {}
2797 config_all_disas = {}
2798 config_devices_mak_list = []
2799 config_devices_h = {}
2800 config_target_h = {}
2801 config_target_mak = {}
2804 'alpha' : ['CONFIG_ALPHA_DIS'],
2805 'avr' : ['CONFIG_AVR_DIS'],
2806 'cris' : ['CONFIG_CRIS_DIS'],
2807 'hexagon' : ['CONFIG_HEXAGON_DIS'],
2808 'hppa' : ['CONFIG_HPPA_DIS'],
2809 'i386' : ['CONFIG_I386_DIS'],
2810 'x86_64' : ['CONFIG_I386_DIS'],
2811 'm68k' : ['CONFIG_M68K_DIS'],
2812 'microblaze' : ['CONFIG_MICROBLAZE_DIS'],
2813 'mips' : ['CONFIG_MIPS_DIS'],
2814 'nios2' : ['CONFIG_NIOS2_DIS'],
2815 'or1k' : ['CONFIG_OPENRISC_DIS'],
2816 'ppc' : ['CONFIG_PPC_DIS'],
2817 'riscv' : ['CONFIG_RISCV_DIS'],
2818 'rx' : ['CONFIG_RX_DIS'],
2819 's390' : ['CONFIG_S390_DIS'],
2820 'sh4' : ['CONFIG_SH4_DIS'],
2821 'sparc' : ['CONFIG_SPARC_DIS'],
2822 'xtensa' : ['CONFIG_XTENSA_DIS'],
2823 'loongarch' : ['CONFIG_LOONGARCH_DIS'],
2826 have_ivshmem = config_host_data.get('CONFIG_EVENTFD')
2828 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \
2829 (have_tpm ? ['CONFIG_TPM=y'] : []) + \
2830 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \
2831 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \
2832 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \
2833 (x11.found() ? ['CONFIG_X11=y'] : []) + \
2834 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \
2835 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \
2836 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \
2837 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \
2838 ('CONFIG_LINUX' in config_host ? ['CONFIG_LINUX=y'] : []) + \
2839 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \
2840 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \
2841 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : [])
2843 ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ]
2845 default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host
2846 actual_target_dirs = []
2848 foreach target : target_dirs
2849 config_target = { 'TARGET_NAME': target.split('-')[0] }
2850 if target.endswith('linux-user')
2851 if targetos != 'linux'
2855 error('Target @0@ is only available on a Linux host'.format(target))
2857 config_target += { 'CONFIG_LINUX_USER': 'y' }
2858 elif target.endswith('bsd-user')
2859 if 'CONFIG_BSD' not in config_host
2863 error('Target @0@ is only available on a BSD host'.format(target))
2865 config_target += { 'CONFIG_BSD_USER': 'y' }
2866 elif target.endswith('softmmu')
2867 config_target += { 'CONFIG_SYSTEM_ONLY': 'y' }
2868 config_target += { 'CONFIG_SOFTMMU': 'y' }
2870 if target.endswith('-user')
2872 'CONFIG_USER_ONLY': 'y',
2873 'CONFIG_QEMU_INTERP_PREFIX':
2874 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME'])
2879 foreach sym: accelerators
2880 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, [])
2881 config_target += { sym: 'y' }
2882 config_all += { sym: 'y' }
2883 if target in modular_tcg
2884 config_target += { 'CONFIG_TCG_MODULAR': 'y' }
2886 config_target += { 'CONFIG_TCG_BUILTIN': 'y' }
2888 accel_kconfig += [ sym + '=y' ]
2891 if accel_kconfig.length() == 0
2895 error('No accelerator available for target @0@'.format(target))
2898 actual_target_dirs += target
2899 config_target += keyval.load('configs/targets' / target + '.mak')
2900 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' }
2902 if 'TARGET_NEED_FDT' in config_target
2903 fdt_required += target
2907 if 'TARGET_BASE_ARCH' not in config_target
2908 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']}
2910 if 'TARGET_ABI_DIR' not in config_target
2911 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']}
2913 if 'TARGET_BIG_ENDIAN' not in config_target
2914 config_target += {'TARGET_BIG_ENDIAN': 'n'}
2917 foreach k, v: disassemblers
2918 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k)
2920 config_target += { sym: 'y' }
2921 config_all_disas += { sym: 'y' }
2926 config_target_data = configuration_data()
2927 foreach k, v: config_target
2928 if not k.startswith('TARGET_') and not k.startswith('CONFIG_')
2930 elif ignored.contains(k)
2932 elif k == 'TARGET_BASE_ARCH'
2933 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is
2934 # not used to select files from sourcesets.
2935 config_target_data.set('TARGET_' + v.to_upper(), 1)
2936 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX'
2937 config_target_data.set_quoted(k, v)
2939 config_target_data.set(k, 1)
2941 config_target_data.set(k, 0)
2943 config_target_data.set(k, v)
2946 config_target_data.set('QEMU_ARCH',
2947 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper())
2948 config_target_h += {target: configure_file(output: target + '-config-target.h',
2949 configuration: config_target_data)}
2951 if target.endswith('-softmmu')
2952 config_input = meson.get_external_property(target, 'default')
2953 config_devices_mak = target + '-config-devices.mak'
2954 config_devices_mak = configure_file(
2955 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'],
2956 output: config_devices_mak,
2957 depfile: config_devices_mak + '.d',
2959 command: [minikconf,
2960 get_option('default_devices') ? '--defconfig' : '--allnoconfig',
2961 config_devices_mak, '@DEPFILE@', '@INPUT@',
2962 host_kconfig, accel_kconfig,
2963 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y'])
2965 config_devices_data = configuration_data()
2966 config_devices = keyval.load(config_devices_mak)
2967 foreach k, v: config_devices
2968 config_devices_data.set(k, 1)
2970 config_devices_mak_list += config_devices_mak
2971 config_devices_h += {target: configure_file(output: target + '-config-devices.h',
2972 configuration: config_devices_data)}
2973 config_target += config_devices
2974 config_all_devices += config_devices
2976 config_target_mak += {target: config_target}
2978 target_dirs = actual_target_dirs
2980 # This configuration is used to build files that are shared by
2981 # multiple binaries, and then extracted out of the "common"
2982 # static_library target.
2984 # We do not use all_sources()/all_dependencies(), because it would
2985 # build literally all source files, including devices only used by
2986 # targets that are not built for this compilation. The CONFIG_ALL
2987 # pseudo symbol replaces it.
2989 config_all += config_all_devices
2990 config_all += config_host
2991 config_all += config_all_disas
2993 'CONFIG_XEN': xen.found(),
2994 'CONFIG_SYSTEM_ONLY': have_system,
2995 'CONFIG_USER_ONLY': have_user,
2999 target_configs_h = []
3000 foreach target: target_dirs
3001 target_configs_h += config_target_h[target]
3002 target_configs_h += config_devices_h.get(target, [])
3004 genh += custom_target('config-poison.h',
3005 input: [target_configs_h],
3006 output: 'config-poison.h',
3008 command: [find_program('scripts/make-config-poison.sh'),
3015 capstone = not_found
3016 if not get_option('capstone').auto() or have_system or have_user
3017 capstone = dependency('capstone', version: '>=3.0.5',
3018 method: 'pkg-config',
3019 required: get_option('capstone'))
3021 # Some versions of capstone have broken pkg-config file
3022 # that reports a wrong -I path, causing the #include to
3023 # fail later. If the system has such a broken version
3025 if capstone.found() and not cc.compiles('#include <capstone.h>',
3026 dependencies: [capstone])
3027 capstone = not_found
3028 if get_option('capstone').enabled()
3029 error('capstone requested, but it does not appear to work')
3034 libvfio_user_dep = not_found
3035 if have_system and vfio_user_server_allowed
3036 libvfio_user_proj = subproject('libvfio-user', required: true)
3037 libvfio_user_dep = libvfio_user_proj.get_variable('libvfio_user_dep')
3041 fdt_opt = get_option('fdt')
3042 if fdt_required.length() > 0 or fdt_opt == 'enabled'
3043 if fdt_opt == 'disabled'
3044 error('fdt disabled but required by targets ' + ', '.join(fdt_required))
3047 if fdt_opt in ['enabled', 'auto', 'system']
3048 fdt = cc.find_library('fdt', required: fdt_opt == 'system')
3049 if fdt.found() and cc.links('''
3051 #include <libfdt_env.h>
3052 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''',
3055 elif fdt_opt == 'system'
3056 error('system libfdt requested, but it is too old (1.5.1 or newer required)')
3058 fdt_opt = 'internal'
3063 assert(fdt_opt == 'internal')
3064 libfdt_proj = subproject('dtc', required: true,
3065 default_options: ['tools=false', 'yaml=disabled',
3066 'python=disabled', 'default_library=static'])
3067 fdt = libfdt_proj.get_variable('libfdt_dep')
3070 fdt_opt = 'disabled'
3073 config_host_data.set('CONFIG_CAPSTONE', capstone.found())
3074 config_host_data.set('CONFIG_FDT', fdt.found())
3075 config_host_data.set('CONFIG_SLIRP', slirp.found())
3077 #####################
3078 # Generated sources #
3079 #####################
3081 genh += configure_file(output: 'config-host.h', configuration: config_host_data)
3083 hxtool = find_program('scripts/hxtool')
3084 shaderinclude = find_program('scripts/shaderinclude.py')
3085 qapi_gen = find_program('scripts/qapi-gen.py')
3086 qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py',
3087 meson.current_source_dir() / 'scripts/qapi/commands.py',
3088 meson.current_source_dir() / 'scripts/qapi/common.py',
3089 meson.current_source_dir() / 'scripts/qapi/error.py',
3090 meson.current_source_dir() / 'scripts/qapi/events.py',
3091 meson.current_source_dir() / 'scripts/qapi/expr.py',
3092 meson.current_source_dir() / 'scripts/qapi/gen.py',
3093 meson.current_source_dir() / 'scripts/qapi/introspect.py',
3094 meson.current_source_dir() / 'scripts/qapi/main.py',
3095 meson.current_source_dir() / 'scripts/qapi/parser.py',
3096 meson.current_source_dir() / 'scripts/qapi/schema.py',
3097 meson.current_source_dir() / 'scripts/qapi/source.py',
3098 meson.current_source_dir() / 'scripts/qapi/types.py',
3099 meson.current_source_dir() / 'scripts/qapi/visit.py',
3100 meson.current_source_dir() / 'scripts/qapi-gen.py'
3104 python, files('scripts/tracetool.py'),
3105 '--backend=' + ','.join(get_option('trace_backends'))
3107 tracetool_depends = files(
3108 'scripts/tracetool/backend/log.py',
3109 'scripts/tracetool/backend/__init__.py',
3110 'scripts/tracetool/backend/dtrace.py',
3111 'scripts/tracetool/backend/ftrace.py',
3112 'scripts/tracetool/backend/simple.py',
3113 'scripts/tracetool/backend/syslog.py',
3114 'scripts/tracetool/backend/ust.py',
3115 'scripts/tracetool/format/ust_events_c.py',
3116 'scripts/tracetool/format/ust_events_h.py',
3117 'scripts/tracetool/format/__init__.py',
3118 'scripts/tracetool/format/d.py',
3119 'scripts/tracetool/format/simpletrace_stap.py',
3120 'scripts/tracetool/format/c.py',
3121 'scripts/tracetool/format/h.py',
3122 'scripts/tracetool/format/log_stap.py',
3123 'scripts/tracetool/format/stap.py',
3124 'scripts/tracetool/__init__.py',
3125 'scripts/tracetool/vcpu.py'
3128 qemu_version_cmd = [find_program('scripts/qemu-version.sh'),
3129 meson.current_source_dir(),
3130 get_option('pkgversion'), meson.project_version()]
3131 qemu_version = custom_target('qemu-version.h',
3132 output: 'qemu-version.h',
3133 command: qemu_version_cmd,
3135 build_by_default: true,
3136 build_always_stale: true)
3137 genh += qemu_version
3141 ['qemu-options.hx', 'qemu-options.def'],
3142 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'],
3146 ['hmp-commands.hx', 'hmp-commands.h'],
3147 ['hmp-commands-info.hx', 'hmp-commands-info.h'],
3150 foreach d : hx_headers
3151 hxdep += custom_target(d[1],
3155 build_by_default: true, # to be removed when added to a target
3156 command: [hxtool, '-h', '@INPUT0@'])
3164 authz_ss = ss.source_set()
3165 blockdev_ss = ss.source_set()
3166 block_ss = ss.source_set()
3167 chardev_ss = ss.source_set()
3168 common_ss = ss.source_set()
3169 crypto_ss = ss.source_set()
3170 hwcore_ss = ss.source_set()
3171 io_ss = ss.source_set()
3172 qmp_ss = ss.source_set()
3173 qom_ss = ss.source_set()
3174 system_ss = ss.source_set()
3175 specific_fuzz_ss = ss.source_set()
3176 specific_ss = ss.source_set()
3177 stub_ss = ss.source_set()
3178 trace_ss = ss.source_set()
3179 user_ss = ss.source_set()
3180 util_ss = ss.source_set()
3183 qtest_module_ss = ss.source_set()
3184 tcg_module_ss = ss.source_set()
3190 target_softmmu_arch = {}
3191 target_user_arch = {}
3197 # TODO: add each directory to the subdirs from its own meson.build, once
3199 trace_events_subdirs = [
3208 trace_events_subdirs += [ 'linux-user' ]
3211 trace_events_subdirs += [ 'bsd-user' ]
3214 trace_events_subdirs += [
3223 trace_events_subdirs += [
3237 'hw/block/dataplane',
3287 if have_system or have_user
3288 trace_events_subdirs += [
3306 vhost_user = not_found
3307 if targetos == 'linux' and have_vhost_user
3308 libvhost_user = subproject('libvhost-user')
3309 vhost_user = libvhost_user.get_variable('vhost_user_dep')
3312 libvduse = not_found
3314 libvduse_proj = subproject('libvduse')
3315 libvduse = libvduse_proj.get_variable('libvduse_dep')
3318 # NOTE: the trace/ subdirectory needs the qapi_trace_events variable
3319 # that is filled in by qapi/.
3333 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO')
3334 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO')
3337 qom_ss = qom_ss.apply(config_host, strict: false)
3338 libqom = static_library('qom', qom_ss.sources() + genh,
3339 dependencies: [qom_ss.dependencies()],
3341 qom = declare_dependency(link_whole: libqom)
3343 event_loop_base = files('event-loop-base.c')
3344 event_loop_base = static_library('event-loop-base', sources: event_loop_base + genh,
3345 build_by_default: true)
3346 event_loop_base = declare_dependency(link_whole: event_loop_base,
3347 dependencies: [qom])
3349 stub_ss = stub_ss.apply(config_all, strict: false)
3351 util_ss.add_all(trace_ss)
3352 util_ss = util_ss.apply(config_all, strict: false)
3353 libqemuutil = static_library('qemuutil',
3354 sources: util_ss.sources() + stub_ss.sources() + genh,
3355 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman])
3356 qemuutil = declare_dependency(link_with: libqemuutil,
3357 sources: genh + version_res,
3358 dependencies: [event_loop_base])
3360 if have_system or have_user
3361 decodetree = generator(find_program('scripts/decodetree.py'),
3362 output: 'decode-@BASENAME@.c.inc',
3363 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@'])
3364 subdir('libdecnumber')
3381 if config_host_data.get('CONFIG_REPLICATION')
3382 block_ss.add(files('replication.c'))
3389 blockdev_ss.add(files(
3396 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon,
3397 # os-win32.c does not
3398 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c'))
3399 system_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')])
3402 common_ss.add(files('cpus-common.c'))
3403 specific_ss.add(files('cpu.c'))
3407 # Work around a gcc bug/misfeature wherein constant propagation looks
3409 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696
3410 # to guess that a const variable is always zero. Without lto, this is
3411 # impossible, as the alias is restricted to page-vary-common.c. Indeed,
3412 # without lto, not even the alias is required -- we simply use different
3413 # declarations in different compilation units.
3414 pagevary = files('page-vary-common.c')
3415 if get_option('b_lto')
3416 pagevary_flags = ['-fno-lto']
3417 if get_option('cfi')
3418 pagevary_flags += '-fno-sanitize=cfi-icall'
3420 pagevary = static_library('page-vary-common', sources: pagevary + genh,
3421 c_args: pagevary_flags)
3422 pagevary = declare_dependency(link_with: pagevary)
3424 common_ss.add(pagevary)
3425 specific_ss.add(files('page-vary.c'))
3433 subdir('semihosting')
3441 common_user_inc = []
3443 subdir('common-user')
3445 subdir('linux-user')
3447 # needed for fuzzing binaries
3448 subdir('tests/qtest/libqos')
3449 subdir('tests/qtest/fuzz')
3452 tcg_real_module_ss = ss.source_set()
3453 tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss)
3454 specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss)
3455 target_modules += { 'accel' : { 'qtest': qtest_module_ss,
3456 'tcg': tcg_real_module_ss }}
3458 ########################
3459 # Library dependencies #
3460 ########################
3462 modinfo_collect = find_program('scripts/modinfo-collect.py')
3463 modinfo_generate = find_program('scripts/modinfo-generate.py')
3468 foreach d, list : modules
3469 if not (d == 'block' ? have_block : have_system)
3473 foreach m, module_ss : list
3475 module_ss = module_ss.apply(config_all, strict: false)
3476 sl = static_library(d + '-' + m, [genh, module_ss.sources()],
3477 dependencies: [modulecommon, module_ss.dependencies()], pic: true)
3483 if module_ss.sources() != []
3484 # FIXME: Should use sl.extract_all_objects(recursive: true) as
3485 # input. Sources can be used multiple times but objects are
3486 # unique when it comes to lookup in compile_commands.json.
3487 # Depnds on a mesion version with
3488 # https://github.com/mesonbuild/meson/pull/8900
3489 modinfo_files += custom_target(d + '-' + m + '.modinfo',
3490 output: d + '-' + m + '.modinfo',
3491 input: module_ss.sources() + genh,
3493 command: [modinfo_collect, module_ss.sources()])
3497 block_ss.add_all(module_ss)
3499 system_ss.add_all(module_ss)
3505 foreach d, list : target_modules
3506 foreach m, module_ss : list
3508 foreach target : target_dirs
3509 if target.endswith('-softmmu')
3510 config_target = config_target_mak[target]
3511 config_target += config_host
3512 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3513 c_args = ['-DNEED_CPU_H',
3514 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3515 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3516 target_module_ss = module_ss.apply(config_target, strict: false)
3517 if target_module_ss.sources() != []
3518 module_name = d + '-' + m + '-' + config_target['TARGET_NAME']
3519 sl = static_library(module_name,
3520 [genh, target_module_ss.sources()],
3521 dependencies: [modulecommon, target_module_ss.dependencies()],
3522 include_directories: target_inc,
3526 # FIXME: Should use sl.extract_all_objects(recursive: true) too.
3527 modinfo_files += custom_target(module_name + '.modinfo',
3528 output: module_name + '.modinfo',
3529 input: target_module_ss.sources() + genh,
3531 command: [modinfo_collect, '--target', target, target_module_ss.sources()])
3536 specific_ss.add_all(module_ss)
3542 foreach target : target_dirs
3543 if target.endswith('-softmmu')
3544 config_target = config_target_mak[target]
3545 config_devices_mak = target + '-config-devices.mak'
3546 modinfo_src = custom_target('modinfo-' + target + '.c',
3547 output: 'modinfo-' + target + '.c',
3548 input: modinfo_files,
3549 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'],
3552 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src)
3553 modinfo_dep = declare_dependency(link_with: modinfo_lib)
3555 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH']
3556 hw_arch[arch].add(modinfo_dep)
3561 nm = find_program('nm')
3562 undefsym = find_program('scripts/undefsym.py')
3563 block_syms = custom_target('block.syms', output: 'block.syms',
3564 input: [libqemuutil, block_mods],
3566 command: [undefsym, nm, '@INPUT@'])
3567 qemu_syms = custom_target('qemu.syms', output: 'qemu.syms',
3568 input: [libqemuutil, softmmu_mods],
3570 command: [undefsym, nm, '@INPUT@'])
3572 authz_ss = authz_ss.apply(config_host, strict: false)
3573 libauthz = static_library('authz', authz_ss.sources() + genh,
3574 dependencies: [authz_ss.dependencies()],
3576 build_by_default: false)
3578 authz = declare_dependency(link_whole: libauthz,
3581 crypto_ss = crypto_ss.apply(config_host, strict: false)
3582 libcrypto = static_library('crypto', crypto_ss.sources() + genh,
3583 dependencies: [crypto_ss.dependencies()],
3585 build_by_default: false)
3587 crypto = declare_dependency(link_whole: libcrypto,
3588 dependencies: [authz, qom])
3590 io_ss = io_ss.apply(config_host, strict: false)
3591 libio = static_library('io', io_ss.sources() + genh,
3592 dependencies: [io_ss.dependencies()],
3593 link_with: libqemuutil,
3595 build_by_default: false)
3597 io = declare_dependency(link_whole: libio, dependencies: [crypto, qom])
3599 libmigration = static_library('migration', sources: migration_files + genh,
3601 build_by_default: false)
3602 migration = declare_dependency(link_with: libmigration,
3603 dependencies: [zlib, qom, io])
3604 system_ss.add(migration)
3606 block_ss = block_ss.apply(config_host, strict: false)
3607 libblock = static_library('block', block_ss.sources() + genh,
3608 dependencies: block_ss.dependencies(),
3609 link_depends: block_syms,
3611 build_by_default: false)
3613 block = declare_dependency(link_whole: [libblock],
3614 link_args: '@block.syms',
3615 dependencies: [crypto, io])
3617 blockdev_ss = blockdev_ss.apply(config_host, strict: false)
3618 libblockdev = static_library('blockdev', blockdev_ss.sources() + genh,
3619 dependencies: blockdev_ss.dependencies(),
3621 build_by_default: false)
3623 blockdev = declare_dependency(link_whole: [libblockdev],
3624 dependencies: [block, event_loop_base])
3626 qmp_ss = qmp_ss.apply(config_host, strict: false)
3627 libqmp = static_library('qmp', qmp_ss.sources() + genh,
3628 dependencies: qmp_ss.dependencies(),
3630 build_by_default: false)
3632 qmp = declare_dependency(link_whole: [libqmp])
3634 libchardev = static_library('chardev', chardev_ss.sources() + genh,
3636 dependencies: chardev_ss.dependencies(),
3637 build_by_default: false)
3639 chardev = declare_dependency(link_whole: libchardev)
3641 hwcore_ss = hwcore_ss.apply(config_host, strict: false)
3642 libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh,
3644 build_by_default: false)
3645 hwcore = declare_dependency(link_whole: libhwcore)
3646 common_ss.add(hwcore)
3652 emulator_modules = []
3653 foreach m : block_mods + softmmu_mods
3654 emulator_modules += shared_module(m.name(),
3655 build_by_default: true,
3659 install_dir: qemu_moddir)
3661 if emulator_modules.length() > 0
3662 alias_target('modules', emulator_modules)
3665 system_ss.add(authz, blockdev, chardev, crypto, io, qmp)
3666 common_ss.add(qom, qemuutil)
3668 common_ss.add_all(when: 'CONFIG_SYSTEM_ONLY', if_true: [system_ss])
3669 common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss)
3671 common_all = common_ss.apply(config_all, strict: false)
3672 common_all = static_library('common',
3673 build_by_default: false,
3674 sources: common_all.sources() + genh,
3675 include_directories: common_user_inc,
3676 implicit_include_directories: false,
3677 dependencies: common_all.dependencies(),
3680 feature_to_c = find_program('scripts/feature_to_c.sh')
3682 if targetos == 'darwin'
3683 entitlement = find_program('scripts/entitlement.sh')
3687 foreach target : target_dirs
3688 config_target = config_target_mak[target]
3689 target_name = config_target['TARGET_NAME']
3690 target_base_arch = config_target['TARGET_BASE_ARCH']
3691 arch_srcs = [config_target_h[target]]
3693 c_args = ['-DNEED_CPU_H',
3694 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3695 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3696 link_args = emulator_link_args
3698 config_target += config_host
3699 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3700 if targetos == 'linux'
3701 target_inc += include_directories('linux-headers', is_system: true)
3703 if target.endswith('-softmmu')
3704 target_type='system'
3705 t = target_softmmu_arch[target_base_arch].apply(config_target, strict: false)
3706 arch_srcs += t.sources()
3707 arch_deps += t.dependencies()
3709 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch
3710 hw = hw_arch[hw_dir].apply(config_target, strict: false)
3711 arch_srcs += hw.sources()
3712 arch_deps += hw.dependencies()
3714 arch_srcs += config_devices_h[target]
3715 link_args += ['@block.syms', '@qemu.syms']
3717 abi = config_target['TARGET_ABI_DIR']
3719 target_inc += common_user_inc
3720 if target_base_arch in target_user_arch
3721 t = target_user_arch[target_base_arch].apply(config_target, strict: false)
3722 arch_srcs += t.sources()
3723 arch_deps += t.dependencies()
3725 if 'CONFIG_LINUX_USER' in config_target
3726 base_dir = 'linux-user'
3728 if 'CONFIG_BSD_USER' in config_target
3729 base_dir = 'bsd-user'
3730 target_inc += include_directories('bsd-user/' / targetos)
3731 target_inc += include_directories('bsd-user/host/' / host_arch)
3732 dir = base_dir / abi
3733 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c')
3735 target_inc += include_directories(
3739 if 'CONFIG_LINUX_USER' in config_target
3740 dir = base_dir / abi
3741 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c')
3742 if config_target.has_key('TARGET_SYSTBL_ABI')
3744 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'],
3745 extra_args : config_target['TARGET_SYSTBL_ABI'])
3750 if 'TARGET_XML_FILES' in config_target
3751 gdbstub_xml = custom_target(target + '-gdbstub-xml.c',
3752 output: target + '-gdbstub-xml.c',
3753 input: files(config_target['TARGET_XML_FILES'].split()),
3754 command: [feature_to_c, '@INPUT@'],
3756 arch_srcs += gdbstub_xml
3759 t = target_arch[target_base_arch].apply(config_target, strict: false)
3760 arch_srcs += t.sources()
3761 arch_deps += t.dependencies()
3763 target_common = common_ss.apply(config_target, strict: false)
3764 objects = common_all.extract_objects(target_common.sources())
3765 deps = target_common.dependencies()
3767 target_specific = specific_ss.apply(config_target, strict: false)
3768 arch_srcs += target_specific.sources()
3769 arch_deps += target_specific.dependencies()
3771 lib = static_library('qemu-' + target,
3772 sources: arch_srcs + genh,
3773 dependencies: arch_deps,
3775 include_directories: target_inc,
3777 build_by_default: false,
3780 if target.endswith('-softmmu')
3782 'name': 'qemu-system-' + target_name,
3783 'win_subsystem': 'console',
3784 'sources': files('softmmu/main.c'),
3787 if targetos == 'windows' and (sdl.found() or gtk.found())
3789 'name': 'qemu-system-' + target_name + 'w',
3790 'win_subsystem': 'windows',
3791 'sources': files('softmmu/main.c'),
3795 if get_option('fuzzing')
3796 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false)
3798 'name': 'qemu-fuzz-' + target_name,
3799 'win_subsystem': 'console',
3800 'sources': specific_fuzz.sources(),
3801 'dependencies': specific_fuzz.dependencies(),
3806 'name': 'qemu-' + target_name,
3807 'win_subsystem': 'console',
3813 exe_name = exe['name']
3814 if targetos == 'darwin'
3815 exe_name += '-unsigned'
3818 emulator = executable(exe_name, exe['sources'],
3821 dependencies: arch_deps + deps + exe['dependencies'],
3822 objects: lib.extract_all_objects(recursive: true),
3823 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []),
3824 link_args: link_args,
3825 win_subsystem: exe['win_subsystem'])
3827 if targetos == 'darwin'
3828 icon = 'pc-bios/qemu.rsrc'
3829 build_input = [emulator, files(icon)]
3831 get_option('bindir') / exe_name,
3832 meson.current_source_dir() / icon
3834 if 'CONFIG_HVF' in config_target
3835 entitlements = 'accel/hvf/entitlements.plist'
3836 build_input += files(entitlements)
3837 install_input += meson.current_source_dir() / entitlements
3840 emulators += {exe['name'] : custom_target(exe['name'],
3842 output: exe['name'],
3843 command: [entitlement, '@OUTPUT@', '@INPUT@'])
3846 meson.add_install_script(entitlement, '--install',
3847 get_option('bindir') / exe['name'],
3850 emulators += {exe['name']: emulator}
3855 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false},
3856 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true},
3857 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true},
3858 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true},
3860 custom_target(exe['name'] + stp['ext'],
3861 input: trace_events_all,
3862 output: exe['name'] + stp['ext'],
3863 install: stp['install'],
3864 install_dir: get_option('datadir') / 'systemtap/tapset',
3866 tracetool, '--group=all', '--format=' + stp['fmt'],
3867 '--binary=' + stp['bin'],
3868 '--target-name=' + target_name,
3869 '--target-type=' + target_type,
3870 '--probe-prefix=qemu.' + target_type + '.' + target_name,
3871 '@INPUT@', '@OUTPUT@'
3873 depend_files: tracetool_depends)
3879 # Other build targets
3881 if 'CONFIG_PLUGIN' in config_host
3882 install_headers('include/qemu/qemu-plugin.h')
3887 # Don't build qemu-keymap if xkbcommon is not explicitly enabled
3888 # when we don't build tools or system
3889 if xkbcommon.found()
3890 # used for the update-keymaps target, so include rules even if !have_tools
3891 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh,
3892 dependencies: [qemuutil, xkbcommon], install: have_tools)
3896 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep],
3897 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true)
3898 qemu_io = executable('qemu-io', files('qemu-io.c'),
3899 dependencies: [block, qemuutil], install: true)
3900 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'),
3901 dependencies: [blockdev, qemuutil, gnutls, selinux],
3904 subdir('storage-daemon')
3905 subdir('contrib/rdmacm-mux')
3906 subdir('contrib/elf2dmp')
3908 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'),
3909 dependencies: qemuutil,
3913 subdir('contrib/vhost-user-blk')
3914 subdir('contrib/vhost-user-gpu')
3915 subdir('contrib/vhost-user-input')
3916 subdir('contrib/vhost-user-scsi')
3919 if targetos == 'linux'
3920 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'),
3921 dependencies: [qemuutil, libcap_ng],
3923 install_dir: get_option('libexecdir'))
3925 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'),
3926 dependencies: [authz, crypto, io, qom, qemuutil,
3927 libcap_ng, mpathpersist],
3932 subdir('contrib/ivshmem-client')
3933 subdir('contrib/ivshmem-server')
3946 if host_machine.system() == 'windows'
3948 find_program('scripts/nsis.py'),
3950 get_option('prefix'),
3951 meson.current_source_dir(),
3952 glib_pc.get_variable('bindir'),
3955 '-DDISPLAYVERSION=' + meson.project_version(),
3958 nsis_cmd += '-DCONFIG_DOCUMENTATION=y'
3961 nsis_cmd += '-DCONFIG_GTK=y'
3964 nsis = custom_target('nsis',
3965 output: 'qemu-setup-' + meson.project_version() + '.exe',
3966 input: files('qemu.nsi'),
3967 build_always_stale: true,
3968 command: nsis_cmd + ['@INPUT@'])
3969 alias_target('installer', nsis)
3972 #########################
3973 # Configuration summary #
3974 #########################
3978 summary_info += {'Build directory': meson.current_build_dir()}
3979 summary_info += {'Source path': meson.current_source_dir()}
3980 summary_info += {'Download dependencies': get_option('wrap_mode') != 'nodownload'}
3981 summary(summary_info, bool_yn: true, section: 'Build environment')
3984 summary_info += {'Install prefix': get_option('prefix')}
3985 summary_info += {'BIOS directory': qemu_datadir}
3986 pathsep = targetos == 'windows' ? ';' : ':'
3987 summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))}
3988 summary_info += {'binary directory': get_option('prefix') / get_option('bindir')}
3989 summary_info += {'library directory': get_option('prefix') / get_option('libdir')}
3990 summary_info += {'module directory': qemu_moddir}
3991 summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')}
3992 summary_info += {'include directory': get_option('prefix') / get_option('includedir')}
3993 summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')}
3994 if targetos != 'windows'
3995 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')}
3996 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')}
3998 summary_info += {'local state directory': 'queried at runtime'}
4000 summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')}
4001 summary(summary_info, bool_yn: true, section: 'Directories')
4005 summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())}
4006 summary_info += {'sphinx-build': sphinx_build}
4007 if config_host.has_key('HAVE_GDB_BIN')
4008 summary_info += {'gdb': config_host['HAVE_GDB_BIN']}
4010 summary_info += {'iasl': iasl}
4011 summary_info += {'genisoimage': config_host['GENISOIMAGE']}
4012 if targetos == 'windows' and have_ga
4013 summary_info += {'wixl': wixl}
4015 if slirp.found() and have_system
4016 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false}
4018 summary(summary_info, bool_yn: true, section: 'Host binaries')
4020 # Configurable features
4022 summary_info += {'Documentation': build_docs}
4023 summary_info += {'system-mode emulation': have_system}
4024 summary_info += {'user-mode emulation': have_user}
4025 summary_info += {'block layer': have_block}
4026 summary_info += {'Install blobs': get_option('install_blobs')}
4027 summary_info += {'module support': enable_modules}
4029 summary_info += {'alternative module path': get_option('module_upgrades')}
4031 summary_info += {'fuzzing support': get_option('fuzzing')}
4033 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)}
4035 summary_info += {'Trace backends': ','.join(get_option('trace_backends'))}
4036 if 'simple' in get_option('trace_backends')
4037 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'}
4039 summary_info += {'D-Bus display': dbus_display}
4040 summary_info += {'QOM debugging': get_option('qom_cast_debug')}
4041 summary_info += {'vhost-kernel support': have_vhost_kernel}
4042 summary_info += {'vhost-net support': have_vhost_net}
4043 summary_info += {'vhost-user support': have_vhost_user}
4044 summary_info += {'vhost-user-crypto support': have_vhost_user_crypto}
4045 summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server}
4046 summary_info += {'vhost-vdpa support': have_vhost_vdpa}
4047 summary_info += {'build guest agent': have_ga}
4048 summary(summary_info, bool_yn: true, section: 'Configurable features')
4050 # Compilation information
4052 summary_info += {'host CPU': cpu}
4053 summary_info += {'host endianness': build_machine.endian()}
4054 summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())}
4055 summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())}
4056 if 'cpp' in all_languages
4057 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())}
4059 summary_info += {'C++ compiler': false}
4061 if targetos == 'darwin'
4062 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())}
4064 option_cflags = (get_option('debug') ? ['-g'] : [])
4065 if get_option('optimization') != 'plain'
4066 option_cflags += ['-O' + get_option('optimization')]
4068 summary_info += {'CFLAGS': ' '.join(get_option('c_args') + option_cflags)}
4069 if 'cpp' in all_languages
4070 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args') + option_cflags)}
4072 if targetos == 'darwin'
4073 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args') + option_cflags)}
4075 link_args = get_option('c_link_args')
4076 if link_args.length() > 0
4077 summary_info += {'LDFLAGS': ' '.join(link_args)}
4079 summary_info += {'QEMU_CFLAGS': ' '.join(qemu_common_flags + qemu_cflags)}
4080 if 'cpp' in all_languages
4081 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_common_flags + qemu_cxxflags)}
4083 if 'objc' in all_languages
4084 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_common_flags)}
4086 summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)}
4087 summary_info += {'link-time optimization (LTO)': get_option('b_lto')}
4088 summary_info += {'PIE': get_option('b_pie')}
4089 summary_info += {'static build': get_option('prefer_static')}
4090 summary_info += {'malloc trim support': has_malloc_trim}
4091 summary_info += {'membarrier': have_membarrier}
4092 summary_info += {'debug graph lock': get_option('debug_graph_lock')}
4093 summary_info += {'debug stack usage': get_option('debug_stack_usage')}
4094 summary_info += {'mutex debugging': get_option('debug_mutex')}
4095 summary_info += {'memory allocator': get_option('malloc')}
4096 summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')}
4097 summary_info += {'avx512bw optimization': config_host_data.get('CONFIG_AVX512BW_OPT')}
4098 summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')}
4099 if get_option('gprof')
4100 gprof_info = 'YES (deprecated)'
4102 gprof_info = get_option('gprof')
4104 summary_info += {'gprof': gprof_info}
4105 summary_info += {'gcov': get_option('b_coverage')}
4106 summary_info += {'thread sanitizer': get_option('tsan')}
4107 summary_info += {'CFI support': get_option('cfi')}
4108 if get_option('cfi')
4109 summary_info += {'CFI debug support': get_option('cfi_debug')}
4111 summary_info += {'strip binaries': get_option('strip')}
4112 summary_info += {'sparse': sparse}
4113 summary_info += {'mingw32 support': targetos == 'windows'}
4114 summary(summary_info, bool_yn: true, section: 'Compilation')
4116 # snarf the cross-compilation information for tests
4119 foreach target: target_dirs
4120 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak'
4121 if fs.exists(tcg_mak)
4122 config_cross_tcg = keyval.load(tcg_mak)
4123 if 'CC' in config_cross_tcg
4124 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']}
4130 summary(summary_info, bool_yn: true, section: 'Cross compilers')
4133 # Targets and accelerators
4136 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')}
4137 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')}
4138 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')}
4139 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')}
4140 summary_info += {'Xen support': xen.found()}
4142 summary_info += {'xen ctrl version': xen.version()}
4144 summary_info += {'Xen emulation': config_all.has_key('CONFIG_XEN_EMU')}
4146 summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')}
4147 if config_all.has_key('CONFIG_TCG')
4148 if get_option('tcg_interpreter')
4149 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'}
4151 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)}
4153 summary_info += {'TCG plugins': config_host.has_key('CONFIG_PLUGIN')}
4154 summary_info += {'TCG debug enabled': config_host.has_key('CONFIG_DEBUG_TCG')}
4156 summary_info += {'target list': ' '.join(target_dirs)}
4158 summary_info += {'default devices': get_option('default_devices')}
4159 summary_info += {'out of process emulation': multiprocess_allowed}
4160 summary_info += {'vfio-user server': vfio_user_server_allowed}
4162 summary(summary_info, bool_yn: true, section: 'Targets and accelerators')
4166 summary_info += {'coroutine backend': coroutine_backend}
4167 summary_info += {'coroutine pool': have_coroutine_pool}
4169 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')}
4170 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')}
4171 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')}
4172 summary_info += {'VirtFS (9P) support': have_virtfs}
4173 summary_info += {'VirtFS (9P) Proxy Helper support (deprecated)': have_virtfs_proxy_helper}
4174 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')}
4175 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')}
4176 summary_info += {'bochs support': get_option('bochs').allowed()}
4177 summary_info += {'cloop support': get_option('cloop').allowed()}
4178 summary_info += {'dmg support': get_option('dmg').allowed()}
4179 summary_info += {'qcow v1 support': get_option('qcow1').allowed()}
4180 summary_info += {'vdi support': get_option('vdi').allowed()}
4181 summary_info += {'vhdx support': get_option('vhdx').allowed()}
4182 summary_info += {'vmdk support': get_option('vmdk').allowed()}
4183 summary_info += {'vpc support': get_option('vpc').allowed()}
4184 summary_info += {'vvfat support': get_option('vvfat').allowed()}
4185 summary_info += {'qed support': get_option('qed').allowed()}
4186 summary_info += {'parallels support': get_option('parallels').allowed()}
4187 summary_info += {'FUSE exports': fuse}
4188 summary_info += {'VDUSE block exports': have_vduse_blk_export}
4190 summary(summary_info, bool_yn: true, section: 'Block layer support')
4194 summary_info += {'TLS priority': get_option('tls_priority')}
4195 summary_info += {'GNUTLS support': gnutls}
4197 summary_info += {' GNUTLS crypto': gnutls_crypto.found()}
4199 summary_info += {'libgcrypt': gcrypt}
4200 summary_info += {'nettle': nettle}
4202 summary_info += {' XTS': xts != 'private'}
4204 summary_info += {'AF_ALG support': have_afalg}
4205 summary_info += {'rng-none': get_option('rng_none')}
4206 summary_info += {'Linux keyring': have_keyring}
4207 summary(summary_info, bool_yn: true, section: 'Crypto')
4211 if targetos == 'darwin'
4212 summary_info += {'Cocoa support': cocoa}
4214 summary_info += {'SDL support': sdl}
4215 summary_info += {'SDL image support': sdl_image}
4216 summary_info += {'GTK support': gtk}
4217 summary_info += {'pixman': pixman}
4218 summary_info += {'VTE support': vte}
4219 summary_info += {'PNG support': png}
4220 summary_info += {'VNC support': vnc}
4222 summary_info += {'VNC SASL support': sasl}
4223 summary_info += {'VNC JPEG support': jpeg}
4225 summary_info += {'spice protocol support': spice_protocol}
4226 if spice_protocol.found()
4227 summary_info += {' spice server support': spice}
4229 summary_info += {'curses support': curses}
4230 summary_info += {'brlapi support': brlapi}
4231 summary(summary_info, bool_yn: true, section: 'User interface')
4235 if targetos not in ['darwin', 'haiku', 'windows']
4236 summary_info += {'OSS support': oss}
4237 summary_info += {'sndio support': sndio}
4238 elif targetos == 'darwin'
4239 summary_info += {'CoreAudio support': coreaudio}
4240 elif targetos == 'windows'
4241 summary_info += {'DirectSound support': dsound}
4243 if targetos == 'linux'
4244 summary_info += {'ALSA support': alsa}
4245 summary_info += {'PulseAudio support': pulse}
4247 summary_info += {'PipeWire support': pipewire}
4248 summary_info += {'JACK support': jack}
4249 summary(summary_info, bool_yn: true, section: 'Audio backends')
4253 if targetos == 'darwin'
4254 summary_info += {'vmnet.framework support': vmnet}
4256 summary_info += {'slirp support': slirp}
4257 summary_info += {'vde support': vde}
4258 summary_info += {'netmap support': have_netmap}
4259 summary_info += {'l2tpv3 support': have_l2tpv3}
4260 summary(summary_info, bool_yn: true, section: 'Network backends')
4264 summary_info += {'libtasn1': tasn1}
4265 summary_info += {'PAM': pam}
4266 summary_info += {'iconv support': iconv}
4267 summary_info += {'virgl support': virgl}
4268 summary_info += {'blkio support': blkio}
4269 summary_info += {'curl support': curl}
4270 summary_info += {'Multipath support': mpathpersist}
4271 summary_info += {'Linux AIO support': libaio}
4272 summary_info += {'Linux io_uring support': linux_io_uring}
4273 summary_info += {'ATTR/XATTR support': libattr}
4274 summary_info += {'RDMA support': rdma}
4275 summary_info += {'PVRDMA support': have_pvrdma}
4276 summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt}
4277 summary_info += {'libcap-ng support': libcap_ng}
4278 summary_info += {'bpf support': libbpf}
4279 summary_info += {'rbd support': rbd}
4280 summary_info += {'smartcard support': cacard}
4281 summary_info += {'U2F support': u2f}
4282 summary_info += {'libusb': libusb}
4283 summary_info += {'usb net redir': usbredir}
4284 summary_info += {'OpenGL support (epoxy)': opengl}
4285 summary_info += {'GBM': gbm}
4286 summary_info += {'libiscsi support': libiscsi}
4287 summary_info += {'libnfs support': libnfs}
4288 if targetos == 'windows'
4290 summary_info += {'QGA VSS support': have_qga_vss}
4293 summary_info += {'seccomp support': seccomp}
4294 summary_info += {'GlusterFS support': glusterfs}
4295 summary_info += {'TPM support': have_tpm}
4296 summary_info += {'libssh support': libssh}
4297 summary_info += {'lzo support': lzo}
4298 summary_info += {'snappy support': snappy}
4299 summary_info += {'bzip2 support': libbzip2}
4300 summary_info += {'lzfse support': liblzfse}
4301 summary_info += {'zstd support': zstd}
4302 summary_info += {'NUMA host support': numa}
4303 summary_info += {'capstone': capstone}
4304 summary_info += {'libpmem support': libpmem}
4305 summary_info += {'libdaxctl support': libdaxctl}
4306 summary_info += {'libudev': libudev}
4307 # Dummy dependency, keep .found()
4308 summary_info += {'FUSE lseek': fuse_lseek.found()}
4309 summary_info += {'selinux': selinux}
4310 summary_info += {'libdw': libdw}
4311 summary(summary_info, bool_yn: true, section: 'Dependencies')
4313 if not supported_cpus.contains(cpu)
4315 warning('SUPPORT FOR THIS HOST CPU WILL GO AWAY IN FUTURE RELEASES!')
4317 message('CPU host architecture ' + cpu + ' support is not currently maintained.')
4318 message('The QEMU project intends to remove support for this host CPU in')
4319 message('a future release if nobody volunteers to maintain it and to')
4320 message('provide a build host for our continuous integration setup.')
4321 message('configure has succeeded and you can continue to build, but')
4322 message('if you care about QEMU on this platform you should contact')
4323 message('us upstream at qemu-devel@nongnu.org.')
4326 if not supported_oses.contains(targetos)
4328 warning('WARNING: SUPPORT FOR THIS HOST OS WILL GO AWAY IN FUTURE RELEASES!')
4330 message('Host OS ' + targetos + 'support is not currently maintained.')
4331 message('The QEMU project intends to remove support for this host OS in')
4332 message('a future release if nobody volunteers to maintain it and to')
4333 message('provide a build host for our continuous integration setup.')
4334 message('configure has succeeded and you can continue to build, but')
4335 message('if you care about QEMU on this platform you should contact')
4336 message('us upstream at qemu-devel@nongnu.org.')