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 if compiler.get_id() == 'gcc'
227 qemu_common_flags += '-DOS_OBJECT_USE_OBJC=0'
229 elif targetos == 'sunos'
230 # needed for CMSG_ macros in sys/socket.h
231 qemu_common_flags += '-D_XOPEN_SOURCE=600'
232 # needed for TIOCWIN* defines in termios.h
233 qemu_common_flags += '-D__EXTENSIONS__'
234 elif targetos == 'haiku'
235 qemu_common_flags += ['-DB_USE_POSITIVE_POSIX_ERRORS', '-D_BSD_SOURCE', '-fPIC']
238 # __sync_fetch_and_and requires at least -march=i486. Many toolchains
239 # use i686 as default anyway, but for those that don't, an explicit
240 # specification is necessary
241 if host_arch == 'i386' and not cc.links('''
242 static int sfaa(int *ptr)
244 return __sync_fetch_and_and(ptr, 0);
250 val = __sync_val_compare_and_swap(&val, 0, 1);
254 qemu_common_flags = ['-march=i486'] + qemu_common_flags
257 if get_option('prefer_static')
258 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static'
261 # Meson currently only handles pie as a boolean for now, so if the user
262 # has explicitly disabled PIE we need to extend our cflags.
264 # -no-pie is supposedly a linker flag that has no effect on the compiler
265 # command line, but some distros, that didn't quite know what they were
266 # doing, made local changes to gcc's specs file that turned it into
267 # a compiler command-line flag.
269 # What about linker flags? For a static build, no PIE is implied by -static
270 # which we added above (and if it's not because of the same specs patching,
271 # there's nothing we can do: compilation will fail, report a bug to your
272 # distro and do not use --disable-pie in the meanwhile). For dynamic linking,
273 # instead, we can't add -no-pie because it overrides -shared: the linker then
274 # tries to build an executable instead of a shared library and fails. So
275 # don't add -no-pie anywhere and cross fingers. :(
276 if not get_option('b_pie')
277 qemu_common_flags += cc.get_supported_arguments('-fno-pie', '-no-pie')
280 if not get_option('stack_protector').disabled()
281 stack_protector_probe = '''
282 int main(int argc, char *argv[])
284 char arr[64], *p = arr, *c = argv[argc - 1];
290 have_stack_protector = false
291 foreach arg : ['-fstack-protector-strong', '-fstack-protector-all']
292 # We need to check both a compile and a link, since some compiler
293 # setups fail only on a .c->.o compile and some only at link time
294 if cc.compiles(stack_protector_probe, args: ['-Werror', arg]) and \
295 cc.links(stack_protector_probe, args: ['-Werror', arg])
296 have_stack_protector = true
302 get_option('stack_protector') \
303 .require(have_stack_protector, error_message: 'Stack protector not supported')
306 coroutine_backend = get_option('coroutine_backend')
308 #include <ucontext.h>
309 #ifdef __stub_makecontext
310 #error Ignoring glibc stub makecontext which will always fail
312 int main(void) { makecontext(0, 0, 0); return 0; }'''
314 # On Windows the only valid backend is the Windows specific one.
315 # For POSIX prefer ucontext, but it's not always possible. The fallback
317 supported_backends = []
318 if targetos == 'windows'
319 supported_backends += ['windows']
321 if targetos != 'darwin' and cc.links(ucontext_probe)
322 supported_backends += ['ucontext']
324 supported_backends += ['sigaltstack']
327 if coroutine_backend == 'auto'
328 coroutine_backend = supported_backends[0]
329 elif coroutine_backend not in supported_backends
330 error('"@0@" backend requested but not available. Available backends: @1@' \
331 .format(coroutine_backend, ', '.join(supported_backends)))
334 # Compiles if SafeStack *not* enabled
335 safe_stack_probe = '''
338 #if defined(__has_feature)
339 #if __has_feature(safe_stack)
340 #error SafeStack Enabled
345 if get_option('safe_stack') != not cc.compiles(safe_stack_probe)
346 safe_stack_arg = get_option('safe_stack') ? '-fsanitize=safe-stack' : '-fno-sanitize=safe-stack'
347 if get_option('safe_stack') != not cc.compiles(safe_stack_probe, args: safe_stack_arg)
348 error(get_option('safe_stack') \
349 ? 'SafeStack not supported by your compiler' \
350 : 'Cannot disable SafeStack')
352 qemu_cflags += safe_stack_arg
353 qemu_ldflags += safe_stack_arg
355 if get_option('safe_stack') and coroutine_backend != 'ucontext'
356 error('SafeStack is only supported with the ucontext coroutine backend')
359 if get_option('sanitizers')
360 if cc.has_argument('-fsanitize=address')
361 qemu_cflags = ['-fsanitize=address'] + qemu_cflags
362 qemu_ldflags = ['-fsanitize=address'] + qemu_ldflags
365 # Detect static linking issue with ubsan - https://gcc.gnu.org/bugzilla/show_bug.cgi?id=84285
366 if cc.links('int main(int argc, char **argv) { return argc + 1; }',
367 args: [qemu_ldflags, '-fsanitize=undefined'])
368 qemu_cflags = ['-fsanitize=undefined'] + qemu_cflags
369 qemu_ldflags = ['-fsanitize=undefined'] + qemu_ldflags
373 # Thread sanitizer is, for now, much noisier than the other sanitizers;
374 # keep it separate until that is not the case.
375 if get_option('tsan')
376 if get_option('sanitizers')
377 error('TSAN is not supported with other sanitizers')
379 if not cc.has_function('__tsan_create_fiber',
380 args: '-fsanitize=thread',
381 prefix: '#include <sanitizer/tsan_interface.h>')
382 error('Cannot enable TSAN due to missing fiber annotation interface')
384 qemu_cflags = ['-fsanitize=thread'] + qemu_cflags
385 qemu_ldflags = ['-fsanitize=thread'] + qemu_ldflags
388 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
389 # The combination is known as "full relro", because .got.plt is read-only too.
390 qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now')
392 if targetos == 'windows'
393 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--no-seh', '-Wl,--nxcompat')
394 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--dynamicbase', '-Wl,--high-entropy-va')
397 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
398 if targetos != 'sunos' and not get_option('tsan')
399 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--warn-common')
402 if get_option('fuzzing')
403 # Specify a filter to only instrument code that is directly related to
405 configure_file(output: 'instrumentation-filter',
406 input: 'scripts/oss-fuzz/instrumentation-filter-template',
409 if cc.compiles('int main () { return 0; }',
410 name: '-fsanitize-coverage-allowlist=/dev/null',
411 args: ['-fsanitize-coverage-allowlist=/dev/null',
412 '-fsanitize-coverage=trace-pc'] )
413 qemu_common_flags += ['-fsanitize-coverage-allowlist=instrumentation-filter']
416 if get_option('fuzzing_engine') == ''
417 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the
418 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link
419 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be
420 # unable to bind the fuzzer-related callbacks added by instrumentation.
421 qemu_common_flags += ['-fsanitize=fuzzer-no-link']
422 qemu_ldflags += ['-fsanitize=fuzzer-no-link']
423 # For the actual fuzzer binaries, we need to link against the libfuzzer
424 # library. They need to be configurable, to support OSS-Fuzz
425 fuzz_exe_ldflags = ['-fsanitize=fuzzer']
427 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and
428 # the needed CFLAGS have already been provided
429 fuzz_exe_ldflags = get_option('fuzzing_engine').split()
433 add_global_arguments(qemu_common_flags, native: false, language: all_languages)
434 add_global_link_arguments(qemu_ldflags, native: false, language: all_languages)
436 # Collect warnings that we want to enable
441 '-Wmissing-prototypes',
442 '-Wstrict-prototypes',
444 '-Wold-style-declaration',
445 '-Wold-style-definition',
450 '-Wignored-qualifiers',
454 '-Wexpansion-to-defined',
455 '-Wimplicit-fallthrough=2',
456 '-Wmissing-format-attribute',
457 '-Wno-initializer-overrides',
458 '-Wno-missing-include-dirs',
459 '-Wno-shift-negative-value',
460 '-Wno-string-plus-int',
461 '-Wno-typedef-redefinition',
462 '-Wno-tautological-type-limit-compare',
464 '-Wno-gnu-variable-sized-type-not-at-end',
467 if targetos != 'darwin'
468 warn_flags += ['-Wthread-safety']
471 # Set up C++ compiler flags
473 if 'cpp' in all_languages
474 qemu_cxxflags = ['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'] + qemu_cflags
477 add_project_arguments(qemu_cflags, native: false, language: 'c')
478 add_project_arguments(cc.get_supported_arguments(warn_flags), native: false, language: 'c')
479 if 'cpp' in all_languages
480 add_project_arguments(qemu_cxxflags, native: false, language: 'cpp')
481 add_project_arguments(cxx.get_supported_arguments(warn_flags), native: false, language: 'cpp')
483 if 'objc' in all_languages
484 # Note sanitizer flags are not applied to Objective-C sources!
485 add_project_arguments(objc.get_supported_arguments(warn_flags), native: false, language: 'objc')
487 if targetos == 'linux'
488 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers',
489 '-isystem', 'linux-headers',
490 language: all_languages)
493 add_project_arguments('-iquote', '.',
494 '-iquote', meson.current_source_dir(),
495 '-iquote', meson.current_source_dir() / 'include',
496 language: all_languages)
498 # If a host-specific include directory exists, list that first...
499 host_include = meson.current_source_dir() / 'host/include/'
500 if fs.is_dir(host_include / host_arch)
501 add_project_arguments('-iquote', host_include / host_arch,
502 language: all_languages)
504 # ... followed by the generic fallback.
505 add_project_arguments('-iquote', host_include / 'generic',
506 language: all_languages)
508 sparse = find_program('cgcc', required: get_option('sparse'))
511 command: [find_program('scripts/check_sparse.py'),
512 'compile_commands.json', sparse.full_path(), '-Wbitwise',
513 '-Wno-transparent-union', '-Wno-old-initializer',
514 '-Wno-non-pointer-null'])
517 ###########################################
518 # Target-specific checks and dependencies #
519 ###########################################
522 if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \
525 #include <sys/types.h>
526 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
527 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
529 args: ['-Werror', '-fsanitize=fuzzer'])
530 error('Your compiler does not support -fsanitize=fuzzer')
534 if 'ftrace' in get_option('trace_backends') and targetos != 'linux'
535 error('ftrace is supported only on Linux')
537 if 'syslog' in get_option('trace_backends') and not cc.compiles('''
540 openlog("qemu", LOG_PID, LOG_DAEMON);
541 syslog(LOG_INFO, "configure");
544 error('syslog is not supported on this system')
547 # Miscellaneous Linux-only features
548 get_option('mpath') \
549 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux')
551 multiprocess_allowed = get_option('multiprocess') \
552 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \
555 vfio_user_server_allowed = get_option('vfio_user_server') \
556 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \
559 have_tpm = get_option('tpm') \
560 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \
564 have_vhost_user = get_option('vhost_user') \
565 .disable_auto_if(targetos != 'linux') \
566 .require(targetos != 'windows',
567 error_message: 'vhost-user is not available on Windows').allowed()
568 have_vhost_vdpa = get_option('vhost_vdpa') \
569 .require(targetos == 'linux',
570 error_message: 'vhost-vdpa is only available on Linux').allowed()
571 have_vhost_kernel = get_option('vhost_kernel') \
572 .require(targetos == 'linux',
573 error_message: 'vhost-kernel is only available on Linux').allowed()
574 have_vhost_user_crypto = get_option('vhost_crypto') \
575 .require(have_vhost_user,
576 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed()
578 have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel
580 have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed()
581 have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed()
582 have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed()
583 have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa
585 # Target-specific libraries and flags
586 libm = cc.find_library('m', required: false)
587 threads = dependency('threads')
588 util = cc.find_library('util', required: false)
594 emulator_link_args = []
601 if targetos == 'windows'
602 midl = find_program('midl', required: false)
603 widl = find_program('widl', required: false)
604 pathcch = cc.find_library('pathcch')
605 socket = cc.find_library('ws2_32')
606 winmm = cc.find_library('winmm')
608 win = import('windows')
609 version_res = win.compile_resources('version.rc',
610 depend_files: files('pc-bios/qemu-nsis.ico'),
611 include_directories: include_directories('.'))
613 elif targetos == 'darwin'
614 coref = dependency('appleframeworks', modules: 'CoreFoundation')
615 iokit = dependency('appleframeworks', modules: 'IOKit', required: false)
616 host_dsosuf = '.dylib'
617 elif targetos == 'sunos'
618 socket = [cc.find_library('socket'),
619 cc.find_library('nsl'),
620 cc.find_library('resolv')]
621 elif targetos == 'haiku'
622 socket = [cc.find_library('posix_error_mapper'),
623 cc.find_library('network'),
624 cc.find_library('bsd')]
625 elif targetos == 'openbsd'
626 if get_option('tcg').allowed() and target_dirs.length() > 0
627 # Disable OpenBSD W^X if available
628 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded')
632 # Target-specific configuration of accelerators
634 if get_option('kvm').allowed() and targetos == 'linux'
635 accelerators += 'CONFIG_KVM'
637 if get_option('whpx').allowed() and targetos == 'windows'
638 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64'
639 error('WHPX requires 64-bit host')
640 elif cc.has_header('winhvplatform.h', required: get_option('whpx')) and \
641 cc.has_header('winhvemulation.h', required: get_option('whpx'))
642 accelerators += 'CONFIG_WHPX'
645 if get_option('hvf').allowed()
646 hvf = dependency('appleframeworks', modules: 'Hypervisor',
647 required: get_option('hvf'))
649 accelerators += 'CONFIG_HVF'
652 if targetos == 'netbsd'
653 nvmm = cc.find_library('nvmm', required: get_option('nvmm'))
655 accelerators += 'CONFIG_NVMM'
660 if get_option('tcg').allowed()
661 if host_arch == 'unknown'
662 if not get_option('tcg_interpreter')
663 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu))
665 elif get_option('tcg_interpreter')
666 warning('Use of the TCG interpreter is not recommended on this host')
667 warning('architecture. There is a native TCG execution backend available')
668 warning('which provides substantially better performance and reliability.')
669 warning('It is strongly recommended to remove the --enable-tcg-interpreter')
670 warning('configuration option on this architecture to use the native')
673 if get_option('tcg_interpreter')
675 elif host_arch == 'x86_64'
677 elif host_arch == 'ppc64'
680 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch,
681 language: all_languages)
683 accelerators += 'CONFIG_TCG'
686 if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled()
687 error('KVM not available on this platform')
689 if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled()
690 error('HVF not available on this platform')
692 if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled()
693 error('NVMM not available on this platform')
695 if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled()
696 error('WHPX not available on this platform')
703 # When bumping glib minimum version, please check also whether to increase
704 # the _WIN32_WINNT setting in osdep.h according to the value from glib
705 glib_req_ver = '>=2.56.0'
706 glib_pc = dependency('glib-2.0', version: glib_req_ver, required: true,
707 method: 'pkg-config')
710 gmodule = dependency('gmodule-export-2.0', version: glib_req_ver, required: true,
711 method: 'pkg-config')
712 elif get_option('plugins')
713 gmodule = dependency('gmodule-no-export-2.0', version: glib_req_ver, required: true,
714 method: 'pkg-config')
719 # This workaround is required due to a bug in pkg-config file for glib as it
720 # doesn't define GLIB_STATIC_COMPILATION for pkg-config --static
721 if targetos == 'windows' and get_option('prefer_static')
722 glib_cflags += ['-DGLIB_STATIC_COMPILATION']
725 # Sanity check that the current size_t matches the
726 # size that glib thinks it should be. This catches
727 # problems on multi-arch where people try to build
728 # 32-bit QEMU while pointing at 64-bit glib headers
730 if not cc.compiles('''
734 #define QEMU_BUILD_BUG_ON(x) \
735 typedef char qemu_build_bug_on[(x)?-1:1] __attribute__((unused));
738 QEMU_BUILD_BUG_ON(sizeof(size_t) != GLIB_SIZEOF_SIZE_T);
740 }''', dependencies: glib_pc, args: glib_cflags)
741 error('''sizeof(size_t) doesn't match GLIB_SIZEOF_SIZE_T.
742 You probably need to set PKG_CONFIG_LIBDIR" to point
743 to the right pkg-config files for your build target.''')
746 # Silence clang warnings triggered by glib < 2.57.2
747 if not cc.compiles('''
752 static void foo_free(Foo *f)
756 G_DEFINE_AUTOPTR_CLEANUP_FUNC(Foo, foo_free)
757 int main(void) { return 0; }''', dependencies: glib_pc, args: ['-Wunused-function', '-Werror'])
758 glib_cflags += cc.get_supported_arguments('-Wno-unused-function')
760 glib = declare_dependency(dependencies: [glib_pc, gmodule],
761 compile_args: glib_cflags,
762 version: glib_pc.version())
764 # Check whether glib has gslice, which we have to avoid for correctness.
765 # TODO: remove this check and the corresponding workaround (qtree) when
766 # the minimum supported glib is >= 2.75.3
767 glib_has_gslice = glib.version().version_compare('<2.75.3')
769 # override glib dep to include the above refinements
770 meson.override_dependency('glib-2.0', glib)
772 # The path to glib.h is added to all compilation commands.
773 add_project_dependencies(glib.partial_dependency(compile_args: true, includes: true),
774 native: false, language: all_languages)
777 gdbus_codegen = not_found
778 gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio'
779 if not get_option('gio').auto() or have_system
780 gio = dependency('gio-2.0', required: get_option('gio'),
781 method: 'pkg-config')
782 if gio.found() and not cc.links('''
786 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
788 }''', dependencies: [glib, gio])
789 if get_option('gio').enabled()
790 error('The installed libgio is broken for static linking')
795 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'),
796 required: get_option('gio'))
797 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'),
798 method: 'pkg-config')
799 gio = declare_dependency(dependencies: [gio, gio_unix],
800 version: gio.version())
803 if gdbus_codegen.found() and get_option('cfi')
804 gdbus_codegen = not_found
805 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity'
808 xml_pp = find_program('scripts/xml-preprocess.py')
811 if 'ust' in get_option('trace_backends')
812 lttng = dependency('lttng-ust', required: true, version: '>= 2.1',
813 method: 'pkg-config')
816 if not get_option('pixman').auto() or have_system or have_tools
817 pixman = dependency('pixman-1', required: get_option('pixman'), version:'>=0.21.8',
818 method: 'pkg-config')
820 if not pixman.found() and (have_system or have_tools)
821 error('FIXME: pixman is currently required')
824 zlib = dependency('zlib', required: true)
827 if not get_option('linux_aio').auto() or have_block
828 libaio = cc.find_library('aio', has_headers: ['libaio.h'],
829 required: get_option('linux_aio'))
832 linux_io_uring_test = '''
833 #include <liburing.h>
834 #include <linux/errqueue.h>
836 int main(void) { return 0; }'''
838 linux_io_uring = not_found
839 if not get_option('linux_io_uring').auto() or have_block
840 linux_io_uring = dependency('liburing', version: '>=0.3',
841 required: get_option('linux_io_uring'),
842 method: 'pkg-config')
843 if not cc.links(linux_io_uring_test)
844 linux_io_uring = not_found
849 if not get_option('libnfs').auto() or have_block
850 libnfs = dependency('libnfs', version: '>=1.9.3',
851 required: get_option('libnfs'),
852 method: 'pkg-config')
857 #include <sys/types.h>
858 #ifdef CONFIG_LIBATTR
859 #include <attr/xattr.h>
861 #include <sys/xattr.h>
863 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }'''
866 have_old_libattr = false
867 if get_option('attr').allowed()
868 if cc.links(libattr_test)
869 libattr = declare_dependency()
871 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'],
872 required: get_option('attr'))
873 if libattr.found() and not \
874 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR')
876 if get_option('attr').enabled()
877 error('could not link libattr')
879 warning('could not link libattr, disabling')
882 have_old_libattr = libattr.found()
887 cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'],
888 required: get_option('cocoa'))
890 vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet'))
891 if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h',
892 'VMNET_BRIDGED_MODE',
895 if get_option('vmnet').enabled()
896 error('vmnet.framework API is outdated')
898 warning('vmnet.framework API is outdated, disabling')
903 seccomp_has_sysrawrc = false
904 if not get_option('seccomp').auto() or have_system or have_tools
905 seccomp = dependency('libseccomp', version: '>=2.3.0',
906 required: get_option('seccomp'),
907 method: 'pkg-config')
909 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h',
910 'SCMP_FLTATR_API_SYSRAWRC',
911 dependencies: seccomp)
915 libcap_ng = not_found
916 if not get_option('cap_ng').auto() or have_system or have_tools
917 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'],
918 required: get_option('cap_ng'))
920 if libcap_ng.found() and not cc.links('''
924 capng_capability_to_name(CAPNG_EFFECTIVE);
926 }''', dependencies: libcap_ng)
927 libcap_ng = not_found
928 if get_option('cap_ng').enabled()
929 error('could not link libcap-ng')
931 warning('could not link libcap-ng, disabling')
935 if get_option('xkbcommon').auto() and not have_system and not have_tools
936 xkbcommon = not_found
938 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'),
939 method: 'pkg-config')
943 if not get_option('slirp').auto() or have_system
944 slirp = dependency('slirp', required: get_option('slirp'),
945 method: 'pkg-config')
946 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because
947 # it passes function pointers within libslirp as callbacks for timers.
948 # When using a system-wide shared libslirp, the type information for the
949 # callback is missing and the timer call produces a false positive with CFI.
950 # Do not use the "version" keyword argument to produce a better error.
951 # with control-flow integrity.
952 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7')
953 if get_option('slirp').enabled()
954 error('Control-Flow Integrity requires libslirp 4.7.')
956 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.')
963 if not get_option('vde').auto() or have_system or have_tools
964 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'],
965 required: get_option('vde'))
967 if vde.found() and not cc.links('''
968 #include <libvdeplug.h>
971 struct vde_open_args a = {0, 0, 0};
975 }''', dependencies: vde)
977 if get_option('cap_ng').enabled()
978 error('could not link libvdeplug')
980 warning('could not link libvdeplug, disabling')
985 if not get_option('pa').auto() or (targetos == 'linux' and have_system)
986 pulse = dependency('libpulse', required: get_option('pa'),
987 method: 'pkg-config')
990 if not get_option('alsa').auto() or (targetos == 'linux' and have_system)
991 alsa = dependency('alsa', required: get_option('alsa'),
992 method: 'pkg-config')
995 if not get_option('jack').auto() or have_system
996 jack = dependency('jack', required: get_option('jack'),
997 method: 'pkg-config')
1000 if not get_option('pipewire').auto() or (targetos == 'linux' and have_system)
1001 pipewire = dependency('libpipewire-0.3', version: '>=0.3.60',
1002 required: get_option('pipewire'),
1003 method: 'pkg-config')
1006 if not get_option('sndio').auto() or have_system
1007 sndio = dependency('sndio', required: get_option('sndio'),
1008 method: 'pkg-config')
1011 spice_protocol = not_found
1012 if not get_option('spice_protocol').auto() or have_system
1013 spice_protocol = dependency('spice-protocol', version: '>=0.14.0',
1014 required: get_option('spice_protocol'),
1015 method: 'pkg-config')
1018 if not get_option('spice').auto() or have_system
1019 spice = dependency('spice-server', version: '>=0.14.0',
1020 required: get_option('spice'),
1021 method: 'pkg-config')
1023 spice_headers = spice.partial_dependency(compile_args: true, includes: true)
1025 rt = cc.find_library('rt', required: false)
1027 libiscsi = not_found
1028 if not get_option('libiscsi').auto() or have_block
1029 libiscsi = dependency('libiscsi', version: '>=1.9.0',
1030 required: get_option('libiscsi'),
1031 method: 'pkg-config')
1034 if not get_option('zstd').auto() or have_block
1035 zstd = dependency('libzstd', version: '>=1.4.0',
1036 required: get_option('zstd'),
1037 method: 'pkg-config')
1041 have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found()
1042 if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu
1043 virgl = dependency('virglrenderer',
1044 method: 'pkg-config',
1045 required: get_option('virglrenderer'))
1047 config_host_data.set('HAVE_VIRGL_D3D_INFO_EXT',
1048 cc.has_member('struct virgl_renderer_resource_info_ext', 'd3d_tex2d',
1049 prefix: '#include <virglrenderer.h>',
1050 dependencies: virgl))
1053 rutabaga = not_found
1054 if not get_option('rutabaga_gfx').auto() or have_system or have_vhost_user_gpu
1055 rutabaga = dependency('rutabaga_gfx_ffi',
1056 method: 'pkg-config',
1057 required: get_option('rutabaga_gfx'))
1060 if not get_option('blkio').auto() or have_block
1061 blkio = dependency('blkio',
1062 method: 'pkg-config',
1063 required: get_option('blkio'))
1066 if not get_option('curl').auto() or have_block
1067 curl = dependency('libcurl', version: '>=7.29.0',
1068 method: 'pkg-config',
1069 required: get_option('curl'))
1072 if targetos == 'linux' and (have_system or have_tools)
1073 libudev = dependency('libudev',
1074 method: 'pkg-config',
1075 required: get_option('libudev'))
1078 mpathlibs = [libudev]
1079 mpathpersist = not_found
1080 if targetos == 'linux' and have_tools and get_option('mpath').allowed()
1081 mpath_test_source = '''
1082 #include <libudev.h>
1083 #include <mpath_persist.h>
1084 unsigned mpath_mx_alloc_len = 1024;
1086 static struct config *multipath_conf;
1087 extern struct udev *udev;
1088 extern struct config *get_multipath_config(void);
1089 extern void put_multipath_config(struct config *conf);
1091 struct config *get_multipath_config(void) { return multipath_conf; }
1092 void put_multipath_config(struct config *conf) { }
1095 multipath_conf = mpath_lib_init();
1098 libmpathpersist = cc.find_library('mpathpersist',
1099 required: get_option('mpath'))
1100 if libmpathpersist.found()
1101 mpathlibs += libmpathpersist
1102 if get_option('prefer_static')
1103 mpathlibs += cc.find_library('devmapper',
1104 required: get_option('mpath'))
1106 mpathlibs += cc.find_library('multipath',
1107 required: get_option('mpath'))
1108 foreach lib: mpathlibs
1114 if mpathlibs.length() == 0
1115 msg = 'Dependencies missing for libmpathpersist'
1116 elif cc.links(mpath_test_source, dependencies: mpathlibs)
1117 mpathpersist = declare_dependency(dependencies: mpathlibs)
1119 msg = 'Cannot detect libmpathpersist API'
1121 if not mpathpersist.found()
1122 if get_option('mpath').enabled()
1125 warning(msg + ', disabling')
1133 if have_system and get_option('curses').allowed()
1135 #if defined(__APPLE__) || defined(__OpenBSD__)
1136 #define _XOPEN_SOURCE_EXTENDED 1
1143 setlocale(LC_ALL, "");
1145 addwstr(L"wide chars\n");
1147 add_wch(WACS_DEGREE);
1151 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw']
1152 curses = dependency(curses_dep_list,
1154 method: 'pkg-config')
1155 msg = get_option('curses').enabled() ? 'curses library not found' : ''
1156 curses_compile_args = ['-DNCURSES_WIDECHAR=1']
1158 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses])
1159 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses],
1160 version: curses.version())
1162 msg = 'curses package not usable'
1166 if not curses.found()
1167 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
1168 if targetos != 'windows' and not has_curses_h
1169 message('Trying with /usr/include/ncursesw')
1170 curses_compile_args += ['-I/usr/include/ncursesw']
1171 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
1174 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw'])
1175 foreach curses_libname : curses_libname_list
1176 libcurses = cc.find_library(curses_libname,
1178 if libcurses.found()
1179 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses)
1180 curses = declare_dependency(compile_args: curses_compile_args,
1181 dependencies: [libcurses])
1184 msg = 'curses library not usable'
1190 if get_option('iconv').allowed()
1191 foreach link_args : [ ['-liconv'], [] ]
1192 # Programs will be linked with glib and this will bring in libiconv on FreeBSD.
1193 # We need to use libiconv if available because mixing libiconv's headers with
1194 # the system libc does not work.
1195 # However, without adding glib to the dependencies -L/usr/local/lib will not be
1196 # included in the command line and libiconv will not be found.
1200 iconv_t conv = iconv_open("WCHAR_T", "UCS-2");
1201 return conv != (iconv_t) -1;
1202 }''', args: link_args, dependencies: glib)
1203 iconv = declare_dependency(link_args: link_args, dependencies: glib)
1208 if curses.found() and not iconv.found()
1209 if get_option('iconv').enabled()
1210 error('iconv not available')
1212 msg = 'iconv required for curses UI but not available'
1215 if not curses.found() and msg != ''
1216 if get_option('curses').enabled()
1219 warning(msg + ', disabling')
1225 if not get_option('brlapi').auto() or have_system
1226 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'],
1227 required: get_option('brlapi'))
1228 if brlapi.found() and not cc.links('''
1231 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi)
1233 if get_option('brlapi').enabled()
1234 error('could not link brlapi')
1236 warning('could not link brlapi, disabling')
1242 if not get_option('sdl').auto() or have_system
1243 sdl = dependency('sdl2', required: get_option('sdl'))
1244 sdl_image = not_found
1247 # Some versions of SDL have problems with -Wundef
1248 if not cc.compiles('''
1250 #include <SDL_syswm.h>
1251 int main(int argc, char *argv[]) { return 0; }
1252 ''', dependencies: sdl, args: '-Werror=undef')
1253 sdl = declare_dependency(compile_args: '-Wno-undef',
1255 version: sdl.version())
1257 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'),
1258 method: 'pkg-config')
1260 if get_option('sdl_image').enabled()
1261 error('sdl-image required, but SDL was @0@'.format(
1262 get_option('sdl').disabled() ? 'disabled' : 'not found'))
1264 sdl_image = not_found
1268 if not get_option('rbd').auto() or have_block
1269 librados = cc.find_library('rados', required: get_option('rbd'))
1270 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'],
1271 required: get_option('rbd'))
1272 if librados.found() and librbd.found()
1275 #include <rbd/librbd.h>
1278 rados_create(&cluster, NULL);
1279 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0)
1283 }''', dependencies: [librbd, librados])
1284 rbd = declare_dependency(dependencies: [librbd, librados])
1285 elif get_option('rbd').enabled()
1286 error('librbd >= 1.12.0 required')
1288 warning('librbd >= 1.12.0 not found, disabling')
1293 glusterfs = not_found
1294 glusterfs_ftruncate_has_stat = false
1295 glusterfs_iocb_has_stat = false
1296 if not get_option('glusterfs').auto() or have_block
1297 glusterfs = dependency('glusterfs-api', version: '>=3',
1298 required: get_option('glusterfs'),
1299 method: 'pkg-config')
1300 if glusterfs.found()
1301 glusterfs_ftruncate_has_stat = cc.links('''
1302 #include <glusterfs/api/glfs.h>
1307 /* new glfs_ftruncate() passes two additional args */
1308 return glfs_ftruncate(NULL, 0, NULL, NULL);
1310 ''', dependencies: glusterfs)
1311 glusterfs_iocb_has_stat = cc.links('''
1312 #include <glusterfs/api/glfs.h>
1314 /* new glfs_io_cbk() passes two additional glfs_stat structs */
1316 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
1322 glfs_io_cbk iocb = &glusterfs_iocb;
1323 iocb(NULL, 0 , NULL, NULL, NULL);
1326 ''', dependencies: glusterfs)
1331 if get_option('hv_balloon').allowed() and have_system
1334 #include <gmodule.h>
1338 tree = g_tree_new((GCompareFunc)strcmp);
1339 (void)g_tree_node_first(tree);
1340 g_tree_destroy(tree);
1343 ''', dependencies: glib)
1346 if get_option('hv_balloon').enabled()
1347 error('could not enable hv-balloon, update your glib')
1349 warning('could not find glib support for hv-balloon, disabling')
1355 if not get_option('libssh').auto() or have_block
1356 libssh = dependency('libssh', version: '>=0.8.7',
1357 method: 'pkg-config',
1358 required: get_option('libssh'))
1361 libbzip2 = not_found
1362 if not get_option('bzip2').auto() or have_block
1363 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'],
1364 required: get_option('bzip2'))
1365 if libbzip2.found() and not cc.links('''
1367 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2)
1368 libbzip2 = not_found
1369 if get_option('bzip2').enabled()
1370 error('could not link libbzip2')
1372 warning('could not link libbzip2, disabling')
1377 liblzfse = not_found
1378 if not get_option('lzfse').auto() or have_block
1379 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'],
1380 required: get_option('lzfse'))
1382 if liblzfse.found() and not cc.links('''
1384 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse)
1385 liblzfse = not_found
1386 if get_option('lzfse').enabled()
1387 error('could not link liblzfse')
1389 warning('could not link liblzfse, disabling')
1394 if get_option('oss').allowed() and have_system
1395 if not cc.has_header('sys/soundcard.h')
1397 elif targetos == 'netbsd'
1398 oss = cc.find_library('ossaudio', required: get_option('oss'))
1400 oss = declare_dependency()
1404 if get_option('oss').enabled()
1405 error('OSS not found')
1410 if not get_option('dsound').auto() or (targetos == 'windows' and have_system)
1411 if cc.has_header('dsound.h')
1412 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid'])
1415 if not dsound.found()
1416 if get_option('dsound').enabled()
1417 error('DirectSound not found')
1422 coreaudio = not_found
1423 if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system)
1424 coreaudio = dependency('appleframeworks', modules: 'CoreAudio',
1425 required: get_option('coreaudio'))
1429 if not get_option('opengl').auto() or have_system or have_vhost_user_gpu
1430 epoxy = dependency('epoxy', method: 'pkg-config',
1431 required: get_option('opengl'))
1432 if cc.has_header('epoxy/egl.h', dependencies: epoxy)
1434 elif get_option('opengl').enabled()
1435 error('epoxy/egl.h not found')
1439 if (have_system or have_tools) and (virgl.found() or opengl.found())
1440 gbm = dependency('gbm', method: 'pkg-config', required: false)
1442 have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found()
1445 gnutls_crypto = not_found
1446 if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system)
1447 # For general TLS support our min gnutls matches
1448 # that implied by our platform support matrix
1450 # For the crypto backends, we look for a newer
1453 # Version 3.6.8 is needed to get XTS
1454 # Version 3.6.13 is needed to get PBKDF
1455 # Version 3.6.14 is needed to get HW accelerated XTS
1457 # If newer enough gnutls isn't available, we can
1458 # still use a different crypto backend to satisfy
1459 # the platform support requirements
1460 gnutls_crypto = dependency('gnutls', version: '>=3.6.14',
1461 method: 'pkg-config',
1463 if gnutls_crypto.found()
1464 gnutls = gnutls_crypto
1466 # Our min version if all we need is TLS
1467 gnutls = dependency('gnutls', version: '>=3.5.18',
1468 method: 'pkg-config',
1469 required: get_option('gnutls'))
1473 # We prefer use of gnutls for crypto, unless the options
1474 # explicitly asked for nettle or gcrypt.
1476 # If gnutls isn't available for crypto, then we'll prefer
1477 # gcrypt over nettle for performance reasons.
1483 if get_option('nettle').enabled() and get_option('gcrypt').enabled()
1484 error('Only one of gcrypt & nettle can be enabled')
1487 # Explicit nettle/gcrypt request, so ignore gnutls for crypto
1488 if get_option('nettle').enabled() or get_option('gcrypt').enabled()
1489 gnutls_crypto = not_found
1492 if not gnutls_crypto.found()
1493 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled()
1494 gcrypt = dependency('libgcrypt', version: '>=1.8',
1495 method: 'config-tool',
1496 required: get_option('gcrypt'))
1497 # Debian has removed -lgpg-error from libgcrypt-config
1498 # as it "spreads unnecessary dependencies" which in
1499 # turn breaks static builds...
1500 if gcrypt.found() and get_option('prefer_static')
1501 gcrypt = declare_dependency(dependencies:
1503 cc.find_library('gpg-error', required: true)],
1504 version: gcrypt.version())
1507 if (not get_option('nettle').auto() or have_system) and not gcrypt.found()
1508 nettle = dependency('nettle', version: '>=3.4',
1509 method: 'pkg-config',
1510 required: get_option('nettle'))
1511 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle)
1517 gmp = dependency('gmp', required: false, method: 'pkg-config')
1518 if nettle.found() and gmp.found()
1519 hogweed = dependency('hogweed', version: '>=3.4',
1520 method: 'pkg-config',
1521 required: get_option('nettle'))
1528 have_gtk_clipboard = get_option('gtk_clipboard').enabled()
1530 if not get_option('gtk').auto() or have_system
1531 gtk = dependency('gtk+-3.0', version: '>=3.22.0',
1532 method: 'pkg-config',
1533 required: get_option('gtk'))
1535 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0',
1536 method: 'pkg-config',
1538 gtk = declare_dependency(dependencies: [gtk, gtkx11],
1539 version: gtk.version())
1541 if not get_option('vte').auto() or have_system
1542 vte = dependency('vte-2.91',
1543 method: 'pkg-config',
1544 required: get_option('vte'))
1546 elif have_gtk_clipboard
1547 error('GTK clipboard requested, but GTK not found')
1553 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found())
1556 if get_option('png').allowed() and have_system
1557 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'),
1558 method: 'pkg-config')
1563 if get_option('vnc').allowed() and have_system
1564 vnc = declare_dependency() # dummy dependency
1565 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'),
1566 method: 'pkg-config')
1567 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'],
1568 required: get_option('vnc_sasl'))
1570 sasl = declare_dependency(dependencies: sasl,
1571 compile_args: '-DSTRUCT_IOVEC_DEFINED')
1576 if not get_option('auth_pam').auto() or have_system
1577 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'],
1578 required: get_option('auth_pam'))
1580 if pam.found() and not cc.links('''
1582 #include <security/pam_appl.h>
1584 const char *service_name = "qemu";
1585 const char *user = "frank";
1586 const struct pam_conv pam_conv = { 0 };
1587 pam_handle_t *pamh = NULL;
1588 pam_start(service_name, user, &pam_conv, &pamh);
1590 }''', dependencies: pam)
1592 if get_option('auth_pam').enabled()
1593 error('could not link libpam')
1595 warning('could not link libpam, disabling')
1600 if not get_option('snappy').auto() or have_system
1601 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'],
1602 required: get_option('snappy'))
1604 if snappy.found() and not cc.links('''
1605 #include <snappy-c.h>
1606 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy)
1608 if get_option('snappy').enabled()
1609 error('could not link libsnappy')
1611 warning('could not link libsnappy, disabling')
1616 if not get_option('lzo').auto() or have_system
1617 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'],
1618 required: get_option('lzo'))
1620 if lzo.found() and not cc.links('''
1621 #include <lzo/lzo1x.h>
1622 int main(void) { lzo_version(); return 0; }''', dependencies: lzo)
1624 if get_option('lzo').enabled()
1625 error('could not link liblzo2')
1627 warning('could not link liblzo2, disabling')
1632 if not get_option('numa').auto() or have_system or have_tools
1633 numa = cc.find_library('numa', has_headers: ['numa.h'],
1634 required: get_option('numa'))
1636 if numa.found() and not cc.links('''
1638 int main(void) { return numa_available(); }
1639 ''', dependencies: numa)
1641 if get_option('numa').enabled()
1642 error('could not link numa')
1644 warning('could not link numa, disabling')
1649 if not get_option('rdma').auto() or have_system
1650 libumad = cc.find_library('ibumad', required: get_option('rdma'))
1651 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'],
1652 required: get_option('rdma')),
1653 cc.find_library('ibverbs', required: get_option('rdma')),
1655 rdma = declare_dependency(dependencies: rdma_libs)
1656 foreach lib: rdma_libs
1664 if get_option('xen').enabled() or (get_option('xen').auto() and have_system)
1665 xencontrol = dependency('xencontrol', required: false,
1666 method: 'pkg-config')
1667 if xencontrol.found()
1668 xen_pc = declare_dependency(version: xencontrol.version(),
1671 # disabler: true makes xen_pc.found() return false if any is not found
1672 dependency('xenstore', required: false,
1673 method: 'pkg-config',
1675 dependency('xenforeignmemory', required: false,
1676 method: 'pkg-config',
1678 dependency('xengnttab', required: false,
1679 method: 'pkg-config',
1681 dependency('xenevtchn', required: false,
1682 method: 'pkg-config',
1684 dependency('xendevicemodel', required: false,
1685 method: 'pkg-config',
1687 # optional, no "disabler: true"
1688 dependency('xentoolcore', required: false,
1689 method: 'pkg-config')])
1695 xen_tests = [ '4.11.0', '4.10.0', '4.9.0', '4.8.0', '4.7.1' ]
1697 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1698 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1699 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1700 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1701 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1704 foreach ver: xen_tests
1705 # cache the various library tests to avoid polluting the logs
1707 foreach l: xen_libs[ver]
1708 if l not in xen_deps
1709 xen_deps += { l: cc.find_library(l, required: false) }
1711 xen_test_deps += xen_deps[l]
1714 # Use -D to pick just one of the test programs in scripts/xen-detect.c
1715 xen_version = ver.split('.')
1716 xen_ctrl_version = xen_version[0] + \
1717 ('0' + xen_version[1]).substring(-2) + \
1718 ('0' + xen_version[2]).substring(-2)
1719 if cc.links(files('scripts/xen-detect.c'),
1720 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version,
1721 dependencies: xen_test_deps)
1722 xen = declare_dependency(version: ver, dependencies: xen_test_deps)
1728 accelerators += 'CONFIG_XEN'
1729 elif get_option('xen').enabled()
1730 error('could not compile and link Xen test program')
1733 have_xen_pci_passthrough = get_option('xen_pci_passthrough') \
1734 .require(xen.found(),
1735 error_message: 'Xen PCI passthrough requested but Xen not enabled') \
1736 .require(targetos == 'linux',
1737 error_message: 'Xen PCI passthrough not available on this platform') \
1738 .require(cpu == 'x86' or cpu == 'x86_64',
1739 error_message: 'Xen PCI passthrough not available on this platform') \
1744 if not get_option('smartcard').auto() or have_system
1745 cacard = dependency('libcacard', required: get_option('smartcard'),
1746 version: '>=2.5.1', method: 'pkg-config')
1750 u2f = dependency('u2f-emu', required: get_option('u2f'),
1751 method: 'pkg-config')
1755 canokey = dependency('canokey-qemu', required: get_option('canokey'),
1756 method: 'pkg-config')
1758 usbredir = not_found
1759 if not get_option('usb_redir').auto() or have_system
1760 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'),
1761 version: '>=0.6', method: 'pkg-config')
1764 if not get_option('libusb').auto() or have_system
1765 libusb = dependency('libusb-1.0', required: get_option('libusb'),
1766 version: '>=1.0.13', method: 'pkg-config')
1770 if not get_option('libpmem').auto() or have_system
1771 libpmem = dependency('libpmem', required: get_option('libpmem'),
1772 method: 'pkg-config')
1774 libdaxctl = not_found
1775 if not get_option('libdaxctl').auto() or have_system
1776 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'),
1777 version: '>=57', method: 'pkg-config')
1781 tasn1 = dependency('libtasn1',
1782 method: 'pkg-config')
1784 keyutils = not_found
1785 if not get_option('libkeyutils').auto() or have_block
1786 keyutils = dependency('libkeyutils', required: get_option('libkeyutils'),
1787 method: 'pkg-config')
1790 has_gettid = cc.has_function('gettid')
1793 selinux = dependency('libselinux',
1794 required: get_option('selinux'),
1795 method: 'pkg-config')
1800 if get_option('malloc') == 'system'
1802 get_option('malloc_trim').allowed() and \
1803 cc.has_function('malloc_trim', prefix: '#include <malloc.h>')
1805 has_malloc_trim = false
1806 malloc = cc.find_library(get_option('malloc'), required: true)
1808 if not has_malloc_trim and get_option('malloc_trim').enabled()
1809 if get_option('malloc') == 'system'
1810 error('malloc_trim not available on this platform.')
1812 error('malloc_trim not available with non-libc memory allocator')
1816 gnu_source_prefix = '''
1822 # Check whether the glibc provides STATX_BASIC_STATS
1824 has_statx = cc.has_header_symbol('sys/stat.h', 'STATX_BASIC_STATS', prefix: gnu_source_prefix)
1826 # Check whether statx() provides mount ID information
1828 has_statx_mnt_id = cc.has_header_symbol('sys/stat.h', 'STATX_MNT_ID', prefix: gnu_source_prefix)
1830 have_vhost_user_blk_server = get_option('vhost_user_blk_server') \
1831 .require(targetos == 'linux',
1832 error_message: 'vhost_user_blk_server requires linux') \
1833 .require(have_vhost_user,
1834 error_message: 'vhost_user_blk_server requires vhost-user support') \
1835 .disable_auto_if(not have_tools and not have_system) \
1838 if get_option('fuse').disabled() and get_option('fuse_lseek').enabled()
1839 error('Cannot enable fuse-lseek while fuse is disabled')
1842 fuse = dependency('fuse3', required: get_option('fuse'),
1843 version: '>=3.1', method: 'pkg-config')
1845 fuse_lseek = not_found
1846 if get_option('fuse_lseek').allowed()
1847 if fuse.version().version_compare('>=3.8')
1849 fuse_lseek = declare_dependency()
1850 elif get_option('fuse_lseek').enabled()
1852 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version())
1854 error('fuse-lseek requires libfuse, which was not found')
1859 have_libvduse = (targetos == 'linux')
1860 if get_option('libvduse').enabled()
1861 if targetos != 'linux'
1862 error('libvduse requires linux')
1864 elif get_option('libvduse').disabled()
1865 have_libvduse = false
1868 have_vduse_blk_export = (have_libvduse and targetos == 'linux')
1869 if get_option('vduse_blk_export').enabled()
1870 if targetos != 'linux'
1871 error('vduse_blk_export requires linux')
1872 elif not have_libvduse
1873 error('vduse_blk_export requires libvduse support')
1875 elif get_option('vduse_blk_export').disabled()
1876 have_vduse_blk_export = false
1880 libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config')
1881 if libbpf.found() and not cc.links('''
1882 #include <bpf/libbpf.h>
1885 bpf_object__destroy_skeleton(NULL);
1887 }''', dependencies: libbpf)
1889 if get_option('bpf').enabled()
1890 error('libbpf skeleton test failed')
1892 warning('libbpf skeleton test failed, disabling')
1898 if not get_option('af_xdp').auto() or have_system
1899 libxdp = dependency('libxdp', required: get_option('af_xdp'),
1900 version: '>=1.4.0', method: 'pkg-config')
1905 if not get_option('libdw').auto() or \
1906 (not get_option('prefer_static') and (have_system or have_user))
1907 libdw = dependency('libdw',
1908 method: 'pkg-config',
1909 required: get_option('libdw'))
1916 audio_drivers_selected = []
1918 audio_drivers_available = {
1919 'alsa': alsa.found(),
1920 'coreaudio': coreaudio.found(),
1921 'dsound': dsound.found(),
1922 'jack': jack.found(),
1924 'pa': pulse.found(),
1925 'pipewire': pipewire.found(),
1927 'sndio': sndio.found(),
1929 foreach k, v: audio_drivers_available
1930 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v)
1933 # Default to native drivers first, OSS second, SDL third
1934 audio_drivers_priority = \
1935 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \
1936 (targetos == 'linux' ? [] : [ 'sdl' ])
1937 audio_drivers_default = []
1938 foreach k: audio_drivers_priority
1939 if audio_drivers_available[k]
1940 audio_drivers_default += k
1944 foreach k: get_option('audio_drv_list')
1946 audio_drivers_selected += audio_drivers_default
1947 elif not audio_drivers_available[k]
1948 error('Audio driver "@0@" not available.'.format(k))
1950 audio_drivers_selected += k
1954 config_host_data.set('CONFIG_AUDIO_DRIVERS',
1955 '"' + '", "'.join(audio_drivers_selected) + '", ')
1957 if get_option('cfi')
1959 # Check for dependency on LTO
1960 if not get_option('b_lto')
1961 error('Selected Control-Flow Integrity but LTO is disabled')
1964 error('Selected Control-Flow Integrity is not compatible with modules')
1966 # Check for cfi flags. CFI requires LTO so we can't use
1967 # get_supported_arguments, but need a more complex "compiles" which allows
1969 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall',
1970 args: ['-flto', '-fsanitize=cfi-icall'] )
1971 cfi_flags += '-fsanitize=cfi-icall'
1973 error('-fsanitize=cfi-icall is not supported by the compiler')
1975 if cc.compiles('int main () { return 0; }',
1976 name: '-fsanitize-cfi-icall-generalize-pointers',
1977 args: ['-flto', '-fsanitize=cfi-icall',
1978 '-fsanitize-cfi-icall-generalize-pointers'] )
1979 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers'
1981 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler')
1983 if get_option('cfi_debug')
1984 if cc.compiles('int main () { return 0; }',
1985 name: '-fno-sanitize-trap=cfi-icall',
1986 args: ['-flto', '-fsanitize=cfi-icall',
1987 '-fno-sanitize-trap=cfi-icall'] )
1988 cfi_flags += '-fno-sanitize-trap=cfi-icall'
1990 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler')
1993 add_global_arguments(cfi_flags, native: false, language: all_languages)
1994 add_global_link_arguments(cfi_flags, native: false, language: all_languages)
1997 have_host_block_device = (targetos != 'darwin' or
1998 cc.has_header('IOKit/storage/IOMedia.h'))
2000 dbus_display = get_option('dbus_display') \
2001 .require(gio.version().version_compare('>=2.64'),
2002 error_message: '-display dbus requires glib>=2.64') \
2003 .require(gdbus_codegen.found(),
2004 error_message: gdbus_codegen_error.format('-display dbus')) \
2007 have_virtfs = get_option('virtfs') \
2008 .require(targetos == 'linux' or targetos == 'darwin',
2009 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \
2010 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'),
2011 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \
2012 .require(targetos == 'darwin' or libattr.found(),
2013 error_message: 'virtio-9p (virtfs) on Linux requires libattr-devel') \
2014 .disable_auto_if(not have_tools and not have_system) \
2017 have_virtfs_proxy_helper = get_option('virtfs_proxy_helper') \
2018 .require(targetos != 'darwin', error_message: 'the virtfs proxy helper is incompatible with macOS') \
2019 .require(have_virtfs, error_message: 'the virtfs proxy helper requires that virtfs is enabled') \
2020 .disable_auto_if(not have_tools) \
2021 .require(libcap_ng.found(), error_message: 'the virtfs proxy helper requires libcap-ng') \
2024 if get_option('block_drv_ro_whitelist') == ''
2025 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '')
2027 config_host_data.set('CONFIG_BDRV_RO_WHITELIST',
2028 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ')
2030 if get_option('block_drv_rw_whitelist') == ''
2031 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '')
2033 config_host_data.set('CONFIG_BDRV_RW_WHITELIST',
2034 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ')
2037 foreach k : get_option('trace_backends')
2038 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true)
2040 config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file'))
2041 config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority'))
2043 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path())
2045 config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir'))
2046 config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix'))
2047 config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir)
2048 config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir)
2049 config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir)
2051 qemu_firmwarepath = ''
2052 foreach k : get_option('qemu_firmwarepath')
2053 qemu_firmwarepath += '"' + get_option('prefix') / k + '", '
2055 config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath)
2057 config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir'))
2058 config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir)
2059 config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir'))
2060 config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir'))
2061 config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir)
2062 config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir'))
2065 config_host_data.set('CONFIG_STAMP', run_command(
2066 meson.current_source_dir() / 'scripts/qemu-stamp.py',
2067 meson.project_version(), get_option('pkgversion'), '--',
2068 meson.current_source_dir() / 'configure',
2069 capture: true, check: true).stdout().strip())
2072 have_slirp_smbd = get_option('slirp_smbd') \
2073 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \
2076 smbd_path = get_option('smbd')
2078 smbd_path = (targetos == 'sunos' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd')
2080 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path)
2083 config_host_data.set('HOST_' + host_arch.to_upper(), 1)
2085 if get_option('module_upgrades') and not enable_modules
2086 error('Cannot enable module-upgrades as modules are not enabled')
2088 config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades'))
2090 config_host_data.set('CONFIG_ATTR', libattr.found())
2091 config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools'))
2092 config_host_data.set('CONFIG_BRLAPI', brlapi.found())
2093 config_host_data.set('CONFIG_BSD', targetos in bsd_oses)
2094 config_host_data.set('CONFIG_COCOA', cocoa.found())
2095 config_host_data.set('CONFIG_DARWIN', targetos == 'darwin')
2096 config_host_data.set('CONFIG_FUZZ', get_option('fuzzing'))
2097 config_host_data.set('CONFIG_GCOV', get_option('b_coverage'))
2098 config_host_data.set('CONFIG_LIBUDEV', libudev.found())
2099 config_host_data.set('CONFIG_LINUX', targetos == 'linux')
2100 config_host_data.set('CONFIG_POSIX', targetos != 'windows')
2101 config_host_data.set('CONFIG_WIN32', targetos == 'windows')
2102 config_host_data.set('CONFIG_LZO', lzo.found())
2103 config_host_data.set('CONFIG_MPATH', mpathpersist.found())
2104 config_host_data.set('CONFIG_BLKIO', blkio.found())
2106 config_host_data.set('CONFIG_BLKIO_VHOST_VDPA_FD',
2107 blkio.version().version_compare('>=1.3.0'))
2109 config_host_data.set('CONFIG_CURL', curl.found())
2110 config_host_data.set('CONFIG_CURSES', curses.found())
2111 config_host_data.set('CONFIG_GBM', gbm.found())
2112 config_host_data.set('CONFIG_GIO', gio.found())
2113 config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found())
2114 if glusterfs.found()
2115 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4'))
2116 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5'))
2117 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6'))
2118 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6'))
2119 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat)
2120 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat)
2122 config_host_data.set('CONFIG_GTK', gtk.found())
2123 config_host_data.set('CONFIG_VTE', vte.found())
2124 config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard)
2125 config_host_data.set('CONFIG_HEXAGON_IDEF_PARSER', get_option('hexagon_idef_parser'))
2126 config_host_data.set('CONFIG_LIBATTR', have_old_libattr)
2127 config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found())
2128 config_host_data.set('CONFIG_EBPF', libbpf.found())
2129 config_host_data.set('CONFIG_AF_XDP', libxdp.found())
2130 config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found())
2131 config_host_data.set('CONFIG_LIBISCSI', libiscsi.found())
2132 config_host_data.set('CONFIG_LIBNFS', libnfs.found())
2133 config_host_data.set('CONFIG_LIBSSH', libssh.found())
2134 config_host_data.set('CONFIG_LINUX_AIO', libaio.found())
2135 config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found())
2136 config_host_data.set('CONFIG_LIBPMEM', libpmem.found())
2137 config_host_data.set('CONFIG_MODULES', enable_modules)
2138 config_host_data.set('CONFIG_NUMA', numa.found())
2140 config_host_data.set('HAVE_NUMA_HAS_PREFERRED_MANY',
2141 cc.has_function('numa_has_preferred_many',
2142 dependencies: numa))
2144 config_host_data.set('CONFIG_OPENGL', opengl.found())
2145 config_host_data.set('CONFIG_PLUGIN', get_option('plugins'))
2146 config_host_data.set('CONFIG_RBD', rbd.found())
2147 config_host_data.set('CONFIG_RDMA', rdma.found())
2148 config_host_data.set('CONFIG_RELOCATABLE', get_option('relocatable'))
2149 config_host_data.set('CONFIG_SAFESTACK', get_option('safe_stack'))
2150 config_host_data.set('CONFIG_SDL', sdl.found())
2151 config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found())
2152 config_host_data.set('CONFIG_SECCOMP', seccomp.found())
2154 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc)
2156 config_host_data.set('CONFIG_PIXMAN', pixman.found())
2157 config_host_data.set('CONFIG_SNAPPY', snappy.found())
2158 config_host_data.set('CONFIG_SOLARIS', targetos == 'sunos')
2159 if get_option('tcg').allowed()
2160 config_host_data.set('CONFIG_TCG', 1)
2161 config_host_data.set('CONFIG_TCG_INTERPRETER', tcg_arch == 'tci')
2163 config_host_data.set('CONFIG_TPM', have_tpm)
2164 config_host_data.set('CONFIG_TSAN', get_option('tsan'))
2165 config_host_data.set('CONFIG_USB_LIBUSB', libusb.found())
2166 config_host_data.set('CONFIG_VDE', vde.found())
2167 config_host_data.set('CONFIG_VHOST', have_vhost)
2168 config_host_data.set('CONFIG_VHOST_NET', have_vhost_net)
2169 config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user)
2170 config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa)
2171 config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel)
2172 config_host_data.set('CONFIG_VHOST_USER', have_vhost_user)
2173 config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto)
2174 config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa)
2175 config_host_data.set('CONFIG_VMNET', vmnet.found())
2176 config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server)
2177 config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export)
2178 config_host_data.set('CONFIG_PNG', png.found())
2179 config_host_data.set('CONFIG_VNC', vnc.found())
2180 config_host_data.set('CONFIG_VNC_JPEG', jpeg.found())
2181 config_host_data.set('CONFIG_VNC_SASL', sasl.found())
2182 config_host_data.set('CONFIG_VIRTFS', have_virtfs)
2183 config_host_data.set('CONFIG_VTE', vte.found())
2184 config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found())
2185 config_host_data.set('CONFIG_KEYUTILS', keyutils.found())
2186 config_host_data.set('CONFIG_GETTID', has_gettid)
2187 config_host_data.set('CONFIG_GNUTLS', gnutls.found())
2188 config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found())
2189 config_host_data.set('CONFIG_TASN1', tasn1.found())
2190 config_host_data.set('CONFIG_GCRYPT', gcrypt.found())
2191 config_host_data.set('CONFIG_NETTLE', nettle.found())
2192 config_host_data.set('CONFIG_HOGWEED', hogweed.found())
2193 config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private')
2194 config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim)
2195 config_host_data.set('CONFIG_STATX', has_statx)
2196 config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id)
2197 config_host_data.set('CONFIG_ZSTD', zstd.found())
2198 config_host_data.set('CONFIG_FUSE', fuse.found())
2199 config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found())
2200 config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found())
2201 if spice_protocol.found()
2202 config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0])
2203 config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1])
2204 config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2])
2206 config_host_data.set('CONFIG_SPICE', spice.found())
2207 config_host_data.set('CONFIG_X11', x11.found())
2208 config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display)
2209 config_host_data.set('CONFIG_CFI', get_option('cfi'))
2210 config_host_data.set('CONFIG_SELINUX', selinux.found())
2211 config_host_data.set('CONFIG_XEN_BACKEND', xen.found())
2212 config_host_data.set('CONFIG_LIBDW', libdw.found())
2214 # protect from xen.version() having less than three components
2215 xen_version = xen.version().split('.') + ['0', '0']
2216 xen_ctrl_version = xen_version[0] + \
2217 ('0' + xen_version[1]).substring(-2) + \
2218 ('0' + xen_version[2]).substring(-2)
2219 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version)
2221 config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version()))
2222 config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0])
2223 config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1])
2224 config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2])
2226 config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf)
2227 config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device)
2229 have_coroutine_pool = get_option('coroutine_pool')
2230 if get_option('debug_stack_usage') and have_coroutine_pool
2231 message('Disabling coroutine pool to measure stack usage')
2232 have_coroutine_pool = false
2234 config_host_data.set('CONFIG_COROUTINE_POOL', have_coroutine_pool)
2235 config_host_data.set('CONFIG_DEBUG_GRAPH_LOCK', get_option('debug_graph_lock'))
2236 config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex'))
2237 config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage'))
2238 config_host_data.set('CONFIG_DEBUG_TCG', get_option('debug_tcg'))
2239 config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed())
2240 config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug'))
2241 config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed())
2244 config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h'))
2245 config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h'))
2246 config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h'))
2247 config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h'))
2248 config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h'))
2249 config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h'))
2250 config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h'))
2251 config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h'))
2252 config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h'))
2253 if targetos == 'windows'
2254 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h'))
2258 config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range'))
2259 config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4'))
2260 config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime'))
2261 config_host_data.set('CONFIG_DUP3', cc.has_function('dup3'))
2262 config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate'))
2263 config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate'))
2264 config_host_data.set('CONFIG_GETCPU', cc.has_function('getcpu', prefix: gnu_source_prefix))
2265 config_host_data.set('CONFIG_SCHED_GETCPU', cc.has_function('sched_getcpu', prefix: '#include <sched.h>'))
2266 # Note that we need to specify prefix: here to avoid incorrectly
2267 # thinking that Windows has posix_memalign()
2268 config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>'))
2269 config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc'))
2270 config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc'))
2271 config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign'))
2272 config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll'))
2273 config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>'))
2274 config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np'))
2275 config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile'))
2276 config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare'))
2277 config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs'))
2278 config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range'))
2279 config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create'))
2280 config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range'))
2281 config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs'))
2282 config_host_data.set('HAVE_GLIB_WITH_SLICE_ALLOCATOR', glib_has_gslice)
2283 config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util))
2284 config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul'))
2285 config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>'))
2287 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS',
2288 cc.has_function('rbd_namespace_exists',
2290 prefix: '#include <rbd/librbd.h>'))
2293 config_host_data.set('HAVE_IBV_ADVISE_MR',
2294 cc.has_function('ibv_advise_mr',
2296 prefix: '#include <infiniband/verbs.h>'))
2299 have_asan_fiber = false
2300 if get_option('sanitizers') and \
2301 not cc.has_function('__sanitizer_start_switch_fiber',
2302 args: '-fsanitize=address',
2303 prefix: '#include <sanitizer/asan_interface.h>')
2304 warning('Missing ASAN due to missing fiber annotation interface')
2305 warning('Without code annotation, the report may be inferior.')
2307 have_asan_fiber = true
2309 config_host_data.set('CONFIG_ASAN_IFACE_FIBER', have_asan_fiber)
2312 config_host_data.set('CONFIG_BLKZONED',
2313 cc.has_header_symbol('linux/blkzoned.h', 'BLKOPENZONE'))
2314 config_host_data.set('CONFIG_EPOLL_CREATE1',
2315 cc.has_header_symbol('sys/epoll.h', 'epoll_create1'))
2316 config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE',
2317 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and
2318 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE'))
2319 config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE',
2320 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE'))
2321 config_host_data.set('CONFIG_FIEMAP',
2322 cc.has_header('linux/fiemap.h') and
2323 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP'))
2324 config_host_data.set('CONFIG_GETRANDOM',
2325 cc.has_function('getrandom') and
2326 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK'))
2327 config_host_data.set('CONFIG_INOTIFY',
2328 cc.has_header_symbol('sys/inotify.h', 'inotify_init'))
2329 config_host_data.set('CONFIG_INOTIFY1',
2330 cc.has_header_symbol('sys/inotify.h', 'inotify_init1'))
2331 config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK',
2332 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK'))
2333 config_host_data.set('CONFIG_RTNETLINK',
2334 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN'))
2335 config_host_data.set('CONFIG_SYSMACROS',
2336 cc.has_header_symbol('sys/sysmacros.h', 'makedev'))
2337 config_host_data.set('HAVE_OPTRESET',
2338 cc.has_header_symbol('getopt.h', 'optreset'))
2339 config_host_data.set('HAVE_IPPROTO_MPTCP',
2340 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP'))
2343 config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID',
2344 cc.has_member('struct sigevent', 'sigev_notify_thread_id',
2345 prefix: '#include <signal.h>'))
2346 config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM',
2347 cc.has_member('struct stat', 'st_atim',
2348 prefix: '#include <sys/stat.h>'))
2349 config_host_data.set('HAVE_BLK_ZONE_REP_CAPACITY',
2350 cc.has_member('struct blk_zone', 'capacity',
2351 prefix: '#include <linux/blkzoned.h>'))
2354 config_host_data.set('CONFIG_IOVEC',
2355 cc.has_type('struct iovec',
2356 prefix: '#include <sys/uio.h>'))
2357 config_host_data.set('HAVE_UTMPX',
2358 cc.has_type('struct utmpx',
2359 prefix: '#include <utmpx.h>'))
2361 config_host_data.set('CONFIG_EVENTFD', cc.links('''
2362 #include <sys/eventfd.h>
2363 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }'''))
2364 config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + '''
2367 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
2368 return fdatasync(0);
2370 #error Not supported
2374 has_madvise = cc.links(gnu_source_prefix + '''
2375 #include <sys/types.h>
2376 #include <sys/mman.h>
2378 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''')
2379 missing_madvise_proto = false
2381 # Some platforms (illumos and Solaris before Solaris 11) provide madvise()
2382 # but forget to prototype it. In this case, has_madvise will be true (the
2383 # test program links despite a compile warning). To detect the
2384 # missing-prototype case, we try again with a definitely-bogus prototype.
2385 # This will only compile if the system headers don't provide the prototype;
2386 # otherwise the conflicting prototypes will cause a compiler error.
2387 missing_madvise_proto = cc.links(gnu_source_prefix + '''
2388 #include <sys/types.h>
2389 #include <sys/mman.h>
2391 extern int madvise(int);
2392 int main(void) { return madvise(0); }''')
2394 config_host_data.set('CONFIG_MADVISE', has_madvise)
2395 config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto)
2397 config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + '''
2398 #include <sys/mman.h>
2399 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }'''))
2400 config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + '''
2402 #if !defined(AT_EMPTY_PATH)
2403 # error missing definition
2405 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
2407 config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + '''
2408 #include <sys/mman.h>
2410 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }'''))
2412 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + '''
2413 #include <pthread.h>
2415 static void *f(void *p) { return NULL; }
2419 pthread_create(&thread, 0, f, 0);
2420 pthread_setname_np(thread, "QEMU");
2422 }''', dependencies: threads))
2423 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + '''
2424 #include <pthread.h>
2426 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
2430 pthread_create(&thread, 0, f, 0);
2432 }''', dependencies: threads))
2433 config_host_data.set('CONFIG_PTHREAD_SET_NAME_NP', cc.links(gnu_source_prefix + '''
2434 #include <pthread.h>
2435 #include <pthread_np.h>
2437 static void *f(void *p) { return NULL; }
2441 pthread_create(&thread, 0, f, 0);
2442 pthread_set_name_np(thread, "QEMU");
2444 }''', dependencies: threads))
2445 config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + '''
2446 #include <pthread.h>
2451 pthread_condattr_t attr
2452 pthread_condattr_init(&attr);
2453 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC);
2455 }''', dependencies: threads))
2456 config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + '''
2457 #include <pthread.h>
2459 static void *f(void *p) { return NULL; }
2462 int setsize = CPU_ALLOC_SIZE(64);
2465 pthread_create(&thread, 0, f, 0);
2466 cpuset = CPU_ALLOC(64);
2467 CPU_ZERO_S(setsize, cpuset);
2468 pthread_setaffinity_np(thread, setsize, cpuset);
2469 pthread_getaffinity_np(thread, setsize, cpuset);
2472 }''', dependencies: threads))
2473 config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + '''
2474 #include <sys/signalfd.h>
2476 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }'''))
2477 config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + '''
2485 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
2486 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
2490 config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + '''
2491 #include <sys/mman.h>
2493 return mlockall(MCL_FUTURE);
2497 if get_option('l2tpv3').allowed() and have_system
2498 have_l2tpv3 = cc.has_type('struct mmsghdr',
2499 prefix: gnu_source_prefix + '''
2500 #include <sys/socket.h>
2501 #include <linux/ip.h>''')
2503 config_host_data.set('CONFIG_L2TPV3', have_l2tpv3)
2506 if get_option('netmap').allowed() and have_system
2507 have_netmap = cc.compiles('''
2508 #include <inttypes.h>
2510 #include <net/netmap.h>
2511 #include <net/netmap_user.h>
2512 #if (NETMAP_API < 11) || (NETMAP_API > 15)
2515 int main(void) { return 0; }''')
2516 if not have_netmap and get_option('netmap').enabled()
2517 error('Netmap headers not available')
2520 config_host_data.set('CONFIG_NETMAP', have_netmap)
2522 # Work around a system header bug with some kernel/XFS header
2523 # versions where they both try to define 'struct fsxattr':
2524 # xfs headers will not try to redefine structs from linux headers
2525 # if this macro is set.
2526 config_host_data.set('HAVE_FSXATTR', cc.links('''
2527 #include <linux/fs.h>
2533 # Some versions of Mac OS X incorrectly define SIZE_MAX
2534 config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles('''
2538 return printf("%zu", SIZE_MAX);
2539 }''', args: ['-Werror']))
2541 # See if 64-bit atomic operations are supported.
2542 # Note that without __atomic builtins, we can only
2543 # assume atomic loads/stores max at pointer size.
2544 config_host_data.set('CONFIG_ATOMIC64', cc.links('''
2548 uint64_t x = 0, y = 0;
2549 y = __atomic_load_n(&x, __ATOMIC_RELAXED);
2550 __atomic_store_n(&x, y, __ATOMIC_RELAXED);
2551 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2552 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
2553 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
2557 has_int128_type = cc.compiles('''
2560 int main(void) { b = a; }''')
2561 config_host_data.set('CONFIG_INT128_TYPE', has_int128_type)
2563 has_int128 = has_int128_type and cc.links('''
2572 config_host_data.set('CONFIG_INT128', has_int128)
2575 # "do we have 128-bit atomics which are handled inline and specifically not
2576 # via libatomic". The reason we can't use libatomic is documented in the
2577 # comment starting "GCC is a house divided" in include/qemu/atomic128.h.
2578 # We only care about these operations on 16-byte aligned pointers, so
2579 # force 16-byte alignment of the pointer, which may be greater than
2580 # __alignof(unsigned __int128) for the host.
2581 atomic_test_128 = '''
2582 int main(int ac, char **av) {
2583 __uint128_t *p = __builtin_assume_aligned(av[ac - 1], 16);
2584 p[1] = __atomic_load_n(&p[0], __ATOMIC_RELAXED);
2585 __atomic_store_n(&p[2], p[3], __ATOMIC_RELAXED);
2586 __atomic_compare_exchange_n(&p[4], &p[5], p[6], 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2589 has_atomic128 = cc.links(atomic_test_128)
2591 config_host_data.set('CONFIG_ATOMIC128', has_atomic128)
2593 if not has_atomic128
2594 # Even with __builtin_assume_aligned, the above test may have failed
2595 # without optimization enabled. Try again with optimizations locally
2596 # enabled for the function. See
2597 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=107389
2598 has_atomic128_opt = cc.links('__attribute__((optimize("O1")))' + atomic_test_128)
2599 config_host_data.set('CONFIG_ATOMIC128_OPT', has_atomic128_opt)
2601 if not has_atomic128_opt
2602 config_host_data.set('CONFIG_CMPXCHG128', cc.links('''
2605 __uint128_t x = 0, y = 0;
2606 __sync_val_compare_and_swap_16(&x, y, x);
2614 config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + '''
2615 #include <sys/auxv.h>
2617 return getauxval(AT_HWCAP) == 0;
2620 config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles('''
2621 #include <linux/usbdevice_fs.h>
2623 #ifndef USBDEVFS_GET_CAPABILITIES
2624 #error "USBDEVFS_GET_CAPABILITIES undefined"
2627 #ifndef USBDEVFS_DISCONNECT_CLAIM
2628 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
2631 int main(void) { return 0; }'''))
2633 have_keyring = get_option('keyring') \
2634 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \
2635 .require(cc.compiles('''
2637 #include <asm/unistd.h>
2638 #include <linux/keyctl.h>
2639 #include <sys/syscall.h>
2642 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
2643 }'''), error_message: 'keyctl syscall not available on this system').allowed()
2644 config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring)
2646 have_cpuid_h = cc.links('''
2649 unsigned a, b, c, d;
2650 unsigned max = __get_cpuid_max(0, 0);
2653 __cpuid(1, a, b, c, d);
2657 __cpuid_count(7, 0, a, b, c, d);
2662 config_host_data.set('CONFIG_CPUID_H', have_cpuid_h)
2664 config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \
2665 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \
2666 .require(cc.links('''
2668 #include <immintrin.h>
2669 static int __attribute__((target("avx2"))) bar(void *a) {
2670 __m256i x = *(__m256i *)a;
2671 return _mm256_testz_si256(x, x);
2673 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2674 '''), error_message: 'AVX2 not available').allowed())
2676 config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \
2677 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \
2678 .require(cc.links('''
2680 #include <immintrin.h>
2681 static int __attribute__((target("avx512f"))) bar(void *a) {
2682 __m512i x = *(__m512i *)a;
2683 return _mm512_test_epi64_mask(x, x);
2685 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2686 '''), error_message: 'AVX512F not available').allowed())
2688 config_host_data.set('CONFIG_AVX512BW_OPT', get_option('avx512bw') \
2689 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512BW') \
2690 .require(cc.links('''
2692 #include <immintrin.h>
2693 static int __attribute__((target("avx512bw"))) bar(void *a) {
2695 __m512i res= _mm512_abs_epi8(*x);
2698 int main(int argc, char *argv[]) { return bar(argv[0]); }
2699 '''), error_message: 'AVX512BW not available').allowed())
2701 # For both AArch64 and AArch32, detect if builtins are available.
2702 config_host_data.set('CONFIG_ARM_AES_BUILTIN', cc.compiles('''
2703 #include <arm_neon.h>
2704 #ifndef __ARM_FEATURE_AES
2705 __attribute__((target("+crypto")))
2707 void foo(uint8x16_t *p) { *p = vaesmcq_u8(*p); }
2710 have_pvrdma = get_option('pvrdma') \
2711 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \
2712 .require(cc.compiles(gnu_source_prefix + '''
2713 #include <sys/mman.h>
2718 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
2721 }'''), error_message: 'PVRDMA requires mremap').allowed()
2724 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links('''
2725 #include <infiniband/verbs.h>
2729 struct ibv_pd *pd = NULL;
2735 mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
2741 if get_option('membarrier').disabled()
2742 have_membarrier = false
2743 elif targetos == 'windows'
2744 have_membarrier = true
2745 elif targetos == 'linux'
2746 have_membarrier = cc.compiles('''
2747 #include <linux/membarrier.h>
2748 #include <sys/syscall.h>
2752 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
2753 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
2757 config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \
2758 .require(have_membarrier, error_message: 'membarrier system call not available') \
2761 have_afalg = get_option('crypto_afalg') \
2762 .require(cc.compiles(gnu_source_prefix + '''
2764 #include <sys/types.h>
2765 #include <sys/socket.h>
2766 #include <linux/if_alg.h>
2769 sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
2772 '''), error_message: 'AF_ALG requested but could not be detected').allowed()
2773 config_host_data.set('CONFIG_AF_ALG', have_afalg)
2775 config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol(
2776 'linux/vm_sockets.h', 'AF_VSOCK',
2777 prefix: '#include <sys/socket.h>',
2781 have_vss_sdk = false # old xp/2003 SDK
2782 if targetos == 'windows' and 'cpp' in all_languages
2783 have_vss = cxx.compiles('''
2784 #define __MIDL_user_allocate_free_DEFINED__
2786 int main(void) { return VSS_CTX_BACKUP; }''')
2787 have_vss_sdk = cxx.has_header('vscoordint.h')
2789 config_host_data.set('HAVE_VSS_SDK', have_vss_sdk)
2791 # Older versions of MinGW do not import _lock_file and _unlock_file properly.
2792 # This was fixed for v6.0.0 with commit b48e3ac8969d.
2793 if targetos == 'windows'
2794 config_host_data.set('HAVE__LOCK_FILE', cc.links('''
2800 }''', name: '_lock_file and _unlock_file'))
2803 if targetos == 'windows'
2804 mingw_has_setjmp_longjmp = cc.links('''
2808 * These functions are not available in setjmp header, but may be
2809 * available at link time, from libmingwex.a.
2811 extern int __mingw_setjmp(jmp_buf);
2812 extern void __attribute__((noreturn)) __mingw_longjmp(jmp_buf, int);
2814 __mingw_setjmp(env);
2815 __mingw_longjmp(env, 0);
2817 ''', name: 'mingw setjmp and longjmp')
2819 if cpu == 'aarch64' and not mingw_has_setjmp_longjmp
2820 error('mingw must provide setjmp/longjmp for windows-arm64')
2824 ########################
2825 # Target configuration #
2826 ########################
2828 minikconf = find_program('scripts/minikconf.py')
2830 (targetos == 'windows' ? 'CONFIG_WIN32' : 'CONFIG_POSIX'): 'y'
2832 if targetos == 'darwin'
2833 config_targetos += {'CONFIG_DARWIN': 'y'}
2834 elif targetos == 'linux'
2835 config_targetos += {'CONFIG_LINUX': 'y'}
2837 if targetos in bsd_oses
2838 config_targetos += {'CONFIG_BSD': 'y'}
2842 config_all_devices = {}
2843 config_all_disas = {}
2844 config_devices_mak_list = []
2845 config_devices_h = {}
2846 config_target_h = {}
2847 config_target_mak = {}
2850 'alpha' : ['CONFIG_ALPHA_DIS'],
2851 'avr' : ['CONFIG_AVR_DIS'],
2852 'cris' : ['CONFIG_CRIS_DIS'],
2853 'hexagon' : ['CONFIG_HEXAGON_DIS'],
2854 'hppa' : ['CONFIG_HPPA_DIS'],
2855 'i386' : ['CONFIG_I386_DIS'],
2856 'x86_64' : ['CONFIG_I386_DIS'],
2857 'm68k' : ['CONFIG_M68K_DIS'],
2858 'microblaze' : ['CONFIG_MICROBLAZE_DIS'],
2859 'mips' : ['CONFIG_MIPS_DIS'],
2860 'nios2' : ['CONFIG_NIOS2_DIS'],
2861 'or1k' : ['CONFIG_OPENRISC_DIS'],
2862 'ppc' : ['CONFIG_PPC_DIS'],
2863 'riscv' : ['CONFIG_RISCV_DIS'],
2864 'rx' : ['CONFIG_RX_DIS'],
2865 's390' : ['CONFIG_S390_DIS'],
2866 'sh4' : ['CONFIG_SH4_DIS'],
2867 'sparc' : ['CONFIG_SPARC_DIS'],
2868 'xtensa' : ['CONFIG_XTENSA_DIS'],
2869 'loongarch' : ['CONFIG_LOONGARCH_DIS'],
2872 have_ivshmem = config_host_data.get('CONFIG_EVENTFD')
2874 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \
2875 (have_tpm ? ['CONFIG_TPM=y'] : []) + \
2876 (pixman.found() ? ['CONFIG_PIXMAN=y'] : []) + \
2877 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \
2878 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \
2879 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \
2880 (x11.found() ? ['CONFIG_X11=y'] : []) + \
2881 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \
2882 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \
2883 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \
2884 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \
2885 (targetos == 'linux' ? ['CONFIG_LINUX=y'] : []) + \
2886 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \
2887 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \
2888 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : []) + \
2889 (hv_balloon ? ['CONFIG_HV_BALLOON_POSSIBLE=y'] : [])
2891 ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ]
2893 default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host
2894 actual_target_dirs = []
2896 foreach target : target_dirs
2897 config_target = { 'TARGET_NAME': target.split('-')[0] }
2898 if target.endswith('linux-user')
2899 if targetos != 'linux'
2903 error('Target @0@ is only available on a Linux host'.format(target))
2905 config_target += { 'CONFIG_LINUX_USER': 'y' }
2906 elif target.endswith('bsd-user')
2907 if targetos not in bsd_oses
2911 error('Target @0@ is only available on a BSD host'.format(target))
2913 config_target += { 'CONFIG_BSD_USER': 'y' }
2914 elif target.endswith('softmmu')
2915 config_target += { 'CONFIG_SYSTEM_ONLY': 'y' }
2916 config_target += { 'CONFIG_SOFTMMU': 'y' }
2918 if target.endswith('-user')
2920 'CONFIG_USER_ONLY': 'y',
2921 'CONFIG_QEMU_INTERP_PREFIX':
2922 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME'])
2927 foreach sym: accelerators
2928 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, [])
2929 config_target += { sym: 'y' }
2930 config_all += { sym: 'y' }
2931 if target in modular_tcg
2932 config_target += { 'CONFIG_TCG_MODULAR': 'y' }
2934 config_target += { 'CONFIG_TCG_BUILTIN': 'y' }
2936 accel_kconfig += [ sym + '=y' ]
2939 if accel_kconfig.length() == 0
2943 error('No accelerator available for target @0@'.format(target))
2946 actual_target_dirs += target
2947 config_target += keyval.load('configs/targets' / target + '.mak')
2948 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' }
2950 if 'TARGET_NEED_FDT' in config_target
2951 fdt_required += target
2955 if 'TARGET_BASE_ARCH' not in config_target
2956 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']}
2958 if 'TARGET_ABI_DIR' not in config_target
2959 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']}
2961 if 'TARGET_BIG_ENDIAN' not in config_target
2962 config_target += {'TARGET_BIG_ENDIAN': 'n'}
2965 foreach k, v: disassemblers
2966 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k)
2968 config_target += { sym: 'y' }
2969 config_all_disas += { sym: 'y' }
2974 config_target_data = configuration_data()
2975 foreach k, v: config_target
2976 if not k.startswith('TARGET_') and not k.startswith('CONFIG_')
2978 elif ignored.contains(k)
2980 elif k == 'TARGET_BASE_ARCH'
2981 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is
2982 # not used to select files from sourcesets.
2983 config_target_data.set('TARGET_' + v.to_upper(), 1)
2984 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX'
2985 config_target_data.set_quoted(k, v)
2987 config_target_data.set(k, 1)
2989 config_target_data.set(k, 0)
2991 config_target_data.set(k, v)
2994 config_target_data.set('QEMU_ARCH',
2995 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper())
2996 config_target_h += {target: configure_file(output: target + '-config-target.h',
2997 configuration: config_target_data)}
2999 if target.endswith('-softmmu')
3000 config_input = meson.get_external_property(target, 'default')
3001 config_devices_mak = target + '-config-devices.mak'
3002 config_devices_mak = configure_file(
3003 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'],
3004 output: config_devices_mak,
3005 depfile: config_devices_mak + '.d',
3007 command: [minikconf,
3008 get_option('default_devices') ? '--defconfig' : '--allnoconfig',
3009 config_devices_mak, '@DEPFILE@', '@INPUT@',
3010 host_kconfig, accel_kconfig,
3011 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y'])
3013 config_devices_data = configuration_data()
3014 config_devices = keyval.load(config_devices_mak)
3015 foreach k, v: config_devices
3016 config_devices_data.set(k, 1)
3018 config_devices_mak_list += config_devices_mak
3019 config_devices_h += {target: configure_file(output: target + '-config-devices.h',
3020 configuration: config_devices_data)}
3021 config_target += config_devices
3022 config_all_devices += config_devices
3024 config_target_mak += {target: config_target}
3026 target_dirs = actual_target_dirs
3028 # This configuration is used to build files that are shared by
3029 # multiple binaries, and then extracted out of the "common"
3030 # static_library target.
3032 # We do not use all_sources()/all_dependencies(), because it would
3033 # build literally all source files, including devices only used by
3034 # targets that are not built for this compilation. The CONFIG_ALL
3035 # pseudo symbol replaces it.
3037 config_all += config_all_devices
3038 config_all += config_targetos
3039 config_all += config_all_disas
3041 'CONFIG_XEN': xen.found(),
3042 'CONFIG_SYSTEM_ONLY': have_system,
3043 'CONFIG_USER_ONLY': have_user,
3047 target_configs_h = []
3048 foreach target: target_dirs
3049 target_configs_h += config_target_h[target]
3050 target_configs_h += config_devices_h.get(target, [])
3052 genh += custom_target('config-poison.h',
3053 input: [target_configs_h],
3054 output: 'config-poison.h',
3056 command: [find_program('scripts/make-config-poison.sh'),
3063 capstone = not_found
3064 if not get_option('capstone').auto() or have_system or have_user
3065 capstone = dependency('capstone', version: '>=3.0.5',
3066 method: 'pkg-config',
3067 required: get_option('capstone'))
3069 # Some versions of capstone have broken pkg-config file
3070 # that reports a wrong -I path, causing the #include to
3071 # fail later. If the system has such a broken version
3073 if capstone.found() and not cc.compiles('#include <capstone.h>',
3074 dependencies: [capstone])
3075 capstone = not_found
3076 if get_option('capstone').enabled()
3077 error('capstone requested, but it does not appear to work')
3082 libvfio_user_dep = not_found
3083 if have_system and vfio_user_server_allowed
3084 libvfio_user_proj = subproject('libvfio-user', required: true)
3085 libvfio_user_dep = libvfio_user_proj.get_variable('libvfio_user_dep')
3089 fdt_opt = get_option('fdt')
3090 if fdt_required.length() > 0 or fdt_opt == 'enabled'
3091 if fdt_opt == 'disabled'
3092 error('fdt disabled but required by targets ' + ', '.join(fdt_required))
3095 if fdt_opt in ['enabled', 'auto', 'system']
3096 if get_option('wrap_mode') == 'nodownload'
3099 fdt = cc.find_library('fdt', required: fdt_opt == 'system')
3100 if fdt.found() and cc.links('''
3102 #include <libfdt_env.h>
3103 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''',
3106 elif fdt_opt == 'system'
3107 error('system libfdt requested, but it is too old (1.5.1 or newer required)')
3109 fdt_opt = 'internal'
3114 assert(fdt_opt == 'internal')
3115 libfdt_proj = subproject('dtc', required: true,
3116 default_options: ['tools=false', 'yaml=disabled',
3117 'python=disabled', 'default_library=static'])
3118 fdt = libfdt_proj.get_variable('libfdt_dep')
3121 fdt_opt = 'disabled'
3124 config_host_data.set('CONFIG_CAPSTONE', capstone.found())
3125 config_host_data.set('CONFIG_FDT', fdt.found())
3126 config_host_data.set('CONFIG_SLIRP', slirp.found())
3128 #####################
3129 # Generated sources #
3130 #####################
3132 genh += configure_file(output: 'config-host.h', configuration: config_host_data)
3134 hxtool = find_program('scripts/hxtool')
3135 shaderinclude = find_program('scripts/shaderinclude.py')
3136 qapi_gen = find_program('scripts/qapi-gen.py')
3137 qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py',
3138 meson.current_source_dir() / 'scripts/qapi/commands.py',
3139 meson.current_source_dir() / 'scripts/qapi/common.py',
3140 meson.current_source_dir() / 'scripts/qapi/error.py',
3141 meson.current_source_dir() / 'scripts/qapi/events.py',
3142 meson.current_source_dir() / 'scripts/qapi/expr.py',
3143 meson.current_source_dir() / 'scripts/qapi/gen.py',
3144 meson.current_source_dir() / 'scripts/qapi/introspect.py',
3145 meson.current_source_dir() / 'scripts/qapi/main.py',
3146 meson.current_source_dir() / 'scripts/qapi/parser.py',
3147 meson.current_source_dir() / 'scripts/qapi/schema.py',
3148 meson.current_source_dir() / 'scripts/qapi/source.py',
3149 meson.current_source_dir() / 'scripts/qapi/types.py',
3150 meson.current_source_dir() / 'scripts/qapi/visit.py',
3151 meson.current_source_dir() / 'scripts/qapi-gen.py'
3155 python, files('scripts/tracetool.py'),
3156 '--backend=' + ','.join(get_option('trace_backends'))
3158 tracetool_depends = files(
3159 'scripts/tracetool/backend/log.py',
3160 'scripts/tracetool/backend/__init__.py',
3161 'scripts/tracetool/backend/dtrace.py',
3162 'scripts/tracetool/backend/ftrace.py',
3163 'scripts/tracetool/backend/simple.py',
3164 'scripts/tracetool/backend/syslog.py',
3165 'scripts/tracetool/backend/ust.py',
3166 'scripts/tracetool/format/ust_events_c.py',
3167 'scripts/tracetool/format/ust_events_h.py',
3168 'scripts/tracetool/format/__init__.py',
3169 'scripts/tracetool/format/d.py',
3170 'scripts/tracetool/format/simpletrace_stap.py',
3171 'scripts/tracetool/format/c.py',
3172 'scripts/tracetool/format/h.py',
3173 'scripts/tracetool/format/log_stap.py',
3174 'scripts/tracetool/format/stap.py',
3175 'scripts/tracetool/__init__.py',
3176 'scripts/tracetool/vcpu.py'
3179 qemu_version_cmd = [find_program('scripts/qemu-version.sh'),
3180 meson.current_source_dir(),
3181 get_option('pkgversion'), meson.project_version()]
3182 qemu_version = custom_target('qemu-version.h',
3183 output: 'qemu-version.h',
3184 command: qemu_version_cmd,
3186 build_by_default: true,
3187 build_always_stale: true)
3188 genh += qemu_version
3192 ['qemu-options.hx', 'qemu-options.def'],
3193 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'],
3197 ['hmp-commands.hx', 'hmp-commands.h'],
3198 ['hmp-commands-info.hx', 'hmp-commands-info.h'],
3201 foreach d : hx_headers
3202 hxdep += custom_target(d[1],
3206 command: [hxtool, '-h', '@INPUT0@'])
3214 authz_ss = ss.source_set()
3215 blockdev_ss = ss.source_set()
3216 block_ss = ss.source_set()
3217 chardev_ss = ss.source_set()
3218 common_ss = ss.source_set()
3219 crypto_ss = ss.source_set()
3220 hwcore_ss = ss.source_set()
3221 io_ss = ss.source_set()
3222 qmp_ss = ss.source_set()
3223 qom_ss = ss.source_set()
3224 system_ss = ss.source_set()
3225 specific_fuzz_ss = ss.source_set()
3226 specific_ss = ss.source_set()
3227 stub_ss = ss.source_set()
3228 trace_ss = ss.source_set()
3229 user_ss = ss.source_set()
3230 util_ss = ss.source_set()
3233 qtest_module_ss = ss.source_set()
3234 tcg_module_ss = ss.source_set()
3240 target_system_arch = {}
3241 target_user_arch = {}
3247 # TODO: add each directory to the subdirs from its own meson.build, once
3249 trace_events_subdirs = [
3258 trace_events_subdirs += [ 'linux-user' ]
3261 trace_events_subdirs += [ 'bsd-user' ]
3264 trace_events_subdirs += [
3273 trace_events_subdirs += [
3287 'hw/block/dataplane',
3338 if have_system or have_user
3339 trace_events_subdirs += [
3357 vhost_user = not_found
3358 if targetos == 'linux' and have_vhost_user
3359 libvhost_user = subproject('libvhost-user')
3360 vhost_user = libvhost_user.get_variable('vhost_user_dep')
3363 libvduse = not_found
3365 libvduse_proj = subproject('libvduse')
3366 libvduse = libvduse_proj.get_variable('libvduse_dep')
3369 # NOTE: the trace/ subdirectory needs the qapi_trace_events variable
3370 # that is filled in by qapi/.
3384 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO')
3385 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO')
3388 qom_ss = qom_ss.apply(config_targetos, strict: false)
3389 libqom = static_library('qom', qom_ss.sources() + genh,
3390 dependencies: [qom_ss.dependencies()],
3392 build_by_default: false)
3393 qom = declare_dependency(link_whole: libqom)
3395 event_loop_base = files('event-loop-base.c')
3396 event_loop_base = static_library('event-loop-base',
3397 sources: event_loop_base + genh,
3399 build_by_default: false)
3400 event_loop_base = declare_dependency(link_whole: event_loop_base,
3401 dependencies: [qom])
3403 stub_ss = stub_ss.apply(config_all, strict: false)
3405 util_ss.add_all(trace_ss)
3406 util_ss = util_ss.apply(config_all, strict: false)
3407 libqemuutil = static_library('qemuutil',
3408 build_by_default: false,
3409 sources: util_ss.sources() + stub_ss.sources() + genh,
3410 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman])
3411 qemuutil = declare_dependency(link_with: libqemuutil,
3412 sources: genh + version_res,
3413 dependencies: [event_loop_base])
3415 if have_system or have_user
3416 decodetree = generator(find_program('scripts/decodetree.py'),
3417 output: 'decode-@BASENAME@.c.inc',
3418 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@'])
3419 subdir('libdecnumber')
3436 if config_host_data.get('CONFIG_REPLICATION')
3437 block_ss.add(files('replication.c'))
3444 blockdev_ss.add(files(
3451 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon,
3452 # os-win32.c does not
3453 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c'))
3454 system_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')])
3457 common_ss.add(files('cpu-common.c'))
3458 specific_ss.add(files('cpu-target.c'))
3462 # Work around a gcc bug/misfeature wherein constant propagation looks
3464 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696
3465 # to guess that a const variable is always zero. Without lto, this is
3466 # impossible, as the alias is restricted to page-vary-common.c. Indeed,
3467 # without lto, not even the alias is required -- we simply use different
3468 # declarations in different compilation units.
3469 pagevary = files('page-vary-common.c')
3470 if get_option('b_lto')
3471 pagevary_flags = ['-fno-lto']
3472 if get_option('cfi')
3473 pagevary_flags += '-fno-sanitize=cfi-icall'
3475 pagevary = static_library('page-vary-common', sources: pagevary + genh,
3476 c_args: pagevary_flags)
3477 pagevary = declare_dependency(link_with: pagevary)
3479 common_ss.add(pagevary)
3480 specific_ss.add(files('page-vary-target.c'))
3488 subdir('semihosting')
3496 common_user_inc = []
3498 subdir('common-user')
3500 subdir('linux-user')
3502 # needed for fuzzing binaries
3503 subdir('tests/qtest/libqos')
3504 subdir('tests/qtest/fuzz')
3507 tcg_real_module_ss = ss.source_set()
3508 tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss)
3509 specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss)
3510 target_modules += { 'accel' : { 'qtest': qtest_module_ss,
3511 'tcg': tcg_real_module_ss }}
3513 ########################
3514 # Library dependencies #
3515 ########################
3517 modinfo_collect = find_program('scripts/modinfo-collect.py')
3518 modinfo_generate = find_program('scripts/modinfo-generate.py')
3523 foreach d, list : modules
3524 if not (d == 'block' ? have_block : have_system)
3528 foreach m, module_ss : list
3530 module_ss = module_ss.apply(config_all, strict: false)
3531 sl = static_library(d + '-' + m, [genh, module_ss.sources()],
3532 dependencies: [modulecommon, module_ss.dependencies()], pic: true)
3538 if module_ss.sources() != []
3539 # FIXME: Should use sl.extract_all_objects(recursive: true) as
3540 # input. Sources can be used multiple times but objects are
3541 # unique when it comes to lookup in compile_commands.json.
3542 # Depnds on a mesion version with
3543 # https://github.com/mesonbuild/meson/pull/8900
3544 modinfo_files += custom_target(d + '-' + m + '.modinfo',
3545 output: d + '-' + m + '.modinfo',
3546 input: module_ss.sources() + genh,
3548 command: [modinfo_collect, module_ss.sources()])
3552 block_ss.add_all(module_ss)
3554 system_ss.add_all(module_ss)
3560 foreach d, list : target_modules
3561 foreach m, module_ss : list
3563 foreach target : target_dirs
3564 if target.endswith('-softmmu')
3565 config_target = config_target_mak[target]
3566 config_target += config_targetos
3567 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3568 c_args = ['-DNEED_CPU_H',
3569 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3570 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3571 target_module_ss = module_ss.apply(config_target, strict: false)
3572 if target_module_ss.sources() != []
3573 module_name = d + '-' + m + '-' + config_target['TARGET_NAME']
3574 sl = static_library(module_name,
3575 [genh, target_module_ss.sources()],
3576 dependencies: [modulecommon, target_module_ss.dependencies()],
3577 include_directories: target_inc,
3581 # FIXME: Should use sl.extract_all_objects(recursive: true) too.
3582 modinfo_files += custom_target(module_name + '.modinfo',
3583 output: module_name + '.modinfo',
3584 input: target_module_ss.sources() + genh,
3586 command: [modinfo_collect, '--target', target, target_module_ss.sources()])
3591 specific_ss.add_all(module_ss)
3597 foreach target : target_dirs
3598 if target.endswith('-softmmu')
3599 config_target = config_target_mak[target]
3600 config_devices_mak = target + '-config-devices.mak'
3601 modinfo_src = custom_target('modinfo-' + target + '.c',
3602 output: 'modinfo-' + target + '.c',
3603 input: modinfo_files,
3604 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'],
3607 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src)
3608 modinfo_dep = declare_dependency(link_with: modinfo_lib)
3610 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH']
3611 hw_arch[arch].add(modinfo_dep)
3616 nm = find_program('nm')
3617 undefsym = find_program('scripts/undefsym.py')
3618 block_syms = custom_target('block.syms', output: 'block.syms',
3619 input: [libqemuutil, block_mods],
3621 command: [undefsym, nm, '@INPUT@'])
3622 qemu_syms = custom_target('qemu.syms', output: 'qemu.syms',
3623 input: [libqemuutil, system_mods],
3625 command: [undefsym, nm, '@INPUT@'])
3627 authz_ss = authz_ss.apply(config_targetos, strict: false)
3628 libauthz = static_library('authz', authz_ss.sources() + genh,
3629 dependencies: [authz_ss.dependencies()],
3631 build_by_default: false)
3633 authz = declare_dependency(link_whole: libauthz,
3636 crypto_ss = crypto_ss.apply(config_targetos, strict: false)
3637 libcrypto = static_library('crypto', crypto_ss.sources() + genh,
3638 dependencies: [crypto_ss.dependencies()],
3640 build_by_default: false)
3642 crypto = declare_dependency(link_whole: libcrypto,
3643 dependencies: [authz, qom])
3645 io_ss = io_ss.apply(config_targetos, strict: false)
3646 libio = static_library('io', io_ss.sources() + genh,
3647 dependencies: [io_ss.dependencies()],
3648 link_with: libqemuutil,
3650 build_by_default: false)
3652 io = declare_dependency(link_whole: libio, dependencies: [crypto, qom])
3654 libmigration = static_library('migration', sources: migration_files + genh,
3656 build_by_default: false)
3657 migration = declare_dependency(link_with: libmigration,
3658 dependencies: [zlib, qom, io])
3659 system_ss.add(migration)
3661 block_ss = block_ss.apply(config_targetos, strict: false)
3662 libblock = static_library('block', block_ss.sources() + genh,
3663 dependencies: block_ss.dependencies(),
3664 link_depends: block_syms,
3666 build_by_default: false)
3668 block = declare_dependency(link_whole: [libblock],
3669 link_args: '@block.syms',
3670 dependencies: [crypto, io])
3672 blockdev_ss = blockdev_ss.apply(config_targetos, strict: false)
3673 libblockdev = static_library('blockdev', blockdev_ss.sources() + genh,
3674 dependencies: blockdev_ss.dependencies(),
3676 build_by_default: false)
3678 blockdev = declare_dependency(link_whole: [libblockdev],
3679 dependencies: [block, event_loop_base])
3681 qmp_ss = qmp_ss.apply(config_targetos, strict: false)
3682 libqmp = static_library('qmp', qmp_ss.sources() + genh,
3683 dependencies: qmp_ss.dependencies(),
3685 build_by_default: false)
3687 qmp = declare_dependency(link_whole: [libqmp])
3689 libchardev = static_library('chardev', chardev_ss.sources() + genh,
3691 dependencies: chardev_ss.dependencies(),
3692 build_by_default: false)
3694 chardev = declare_dependency(link_whole: libchardev)
3696 hwcore_ss = hwcore_ss.apply(config_targetos, strict: false)
3697 libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh,
3699 build_by_default: false)
3700 hwcore = declare_dependency(link_whole: libhwcore)
3701 common_ss.add(hwcore)
3707 emulator_modules = []
3708 foreach m : block_mods + system_mods
3709 emulator_modules += shared_module(m.name(),
3710 build_by_default: true,
3714 install_dir: qemu_moddir)
3716 if emulator_modules.length() > 0
3717 alias_target('modules', emulator_modules)
3720 system_ss.add(authz, blockdev, chardev, crypto, io, qmp)
3721 common_ss.add(qom, qemuutil)
3723 common_ss.add_all(when: 'CONFIG_SYSTEM_ONLY', if_true: [system_ss])
3724 common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss)
3726 common_all = common_ss.apply(config_all, strict: false)
3727 common_all = static_library('common',
3728 build_by_default: false,
3729 sources: common_all.sources() + genh,
3730 include_directories: common_user_inc,
3731 implicit_include_directories: false,
3732 dependencies: common_all.dependencies(),
3735 feature_to_c = find_program('scripts/feature_to_c.py')
3737 if targetos == 'darwin'
3738 entitlement = find_program('scripts/entitlement.sh')
3742 foreach target : target_dirs
3743 config_target = config_target_mak[target]
3744 target_name = config_target['TARGET_NAME']
3745 target_base_arch = config_target['TARGET_BASE_ARCH']
3746 arch_srcs = [config_target_h[target]]
3748 c_args = ['-DNEED_CPU_H',
3749 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3750 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3751 link_args = emulator_link_args
3753 config_target += config_targetos
3754 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3755 if targetos == 'linux'
3756 target_inc += include_directories('linux-headers', is_system: true)
3758 if target.endswith('-softmmu')
3759 target_type='system'
3760 t = target_system_arch[target_base_arch].apply(config_target, strict: false)
3761 arch_srcs += t.sources()
3762 arch_deps += t.dependencies()
3764 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch
3765 hw = hw_arch[hw_dir].apply(config_target, strict: false)
3766 arch_srcs += hw.sources()
3767 arch_deps += hw.dependencies()
3769 arch_srcs += config_devices_h[target]
3770 link_args += ['@block.syms', '@qemu.syms']
3772 abi = config_target['TARGET_ABI_DIR']
3774 target_inc += common_user_inc
3775 if target_base_arch in target_user_arch
3776 t = target_user_arch[target_base_arch].apply(config_target, strict: false)
3777 arch_srcs += t.sources()
3778 arch_deps += t.dependencies()
3780 if 'CONFIG_LINUX_USER' in config_target
3781 base_dir = 'linux-user'
3783 if 'CONFIG_BSD_USER' in config_target
3784 base_dir = 'bsd-user'
3785 target_inc += include_directories('bsd-user/' / targetos)
3786 target_inc += include_directories('bsd-user/host/' / host_arch)
3787 dir = base_dir / abi
3788 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c')
3790 target_inc += include_directories(
3794 if 'CONFIG_LINUX_USER' in config_target
3795 dir = base_dir / abi
3796 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c')
3797 if config_target.has_key('TARGET_SYSTBL_ABI')
3799 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'],
3800 extra_args : config_target['TARGET_SYSTBL_ABI'])
3805 if 'TARGET_XML_FILES' in config_target
3806 gdbstub_xml = custom_target(target + '-gdbstub-xml.c',
3807 output: target + '-gdbstub-xml.c',
3808 input: files(config_target['TARGET_XML_FILES'].split()),
3809 command: [feature_to_c, '@INPUT@'],
3811 arch_srcs += gdbstub_xml
3814 t = target_arch[target_base_arch].apply(config_target, strict: false)
3815 arch_srcs += t.sources()
3816 arch_deps += t.dependencies()
3818 target_common = common_ss.apply(config_target, strict: false)
3819 objects = common_all.extract_objects(target_common.sources())
3820 deps = target_common.dependencies()
3822 target_specific = specific_ss.apply(config_target, strict: false)
3823 arch_srcs += target_specific.sources()
3824 arch_deps += target_specific.dependencies()
3826 lib = static_library('qemu-' + target,
3827 sources: arch_srcs + genh,
3828 dependencies: arch_deps,
3830 include_directories: target_inc,
3832 build_by_default: false,
3835 if target.endswith('-softmmu')
3837 'name': 'qemu-system-' + target_name,
3838 'win_subsystem': 'console',
3839 'sources': files('system/main.c'),
3842 if targetos == 'windows' and (sdl.found() or gtk.found())
3844 'name': 'qemu-system-' + target_name + 'w',
3845 'win_subsystem': 'windows',
3846 'sources': files('system/main.c'),
3850 if get_option('fuzzing')
3851 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false)
3853 'name': 'qemu-fuzz-' + target_name,
3854 'win_subsystem': 'console',
3855 'sources': specific_fuzz.sources(),
3856 'dependencies': specific_fuzz.dependencies(),
3861 'name': 'qemu-' + target_name,
3862 'win_subsystem': 'console',
3868 exe_name = exe['name']
3869 if targetos == 'darwin'
3870 exe_name += '-unsigned'
3873 emulator = executable(exe_name, exe['sources'],
3876 dependencies: arch_deps + deps + exe['dependencies'],
3877 objects: lib.extract_all_objects(recursive: true),
3878 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []),
3879 link_args: link_args,
3880 win_subsystem: exe['win_subsystem'])
3882 if targetos == 'darwin'
3883 icon = 'pc-bios/qemu.rsrc'
3884 build_input = [emulator, files(icon)]
3886 get_option('bindir') / exe_name,
3887 meson.current_source_dir() / icon
3889 if 'CONFIG_HVF' in config_target
3890 entitlements = 'accel/hvf/entitlements.plist'
3891 build_input += files(entitlements)
3892 install_input += meson.current_source_dir() / entitlements
3895 emulators += {exe['name'] : custom_target(exe['name'],
3897 output: exe['name'],
3898 command: [entitlement, '@OUTPUT@', '@INPUT@'])
3901 meson.add_install_script(entitlement, '--install',
3902 get_option('bindir') / exe['name'],
3905 emulators += {exe['name']: emulator}
3910 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false},
3911 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true},
3912 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true},
3913 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true},
3915 custom_target(exe['name'] + stp['ext'],
3916 input: trace_events_all,
3917 output: exe['name'] + stp['ext'],
3918 install: stp['install'],
3919 install_dir: get_option('datadir') / 'systemtap/tapset',
3921 tracetool, '--group=all', '--format=' + stp['fmt'],
3922 '--binary=' + stp['bin'],
3923 '--target-name=' + target_name,
3924 '--target-type=' + target_type,
3925 '--probe-prefix=qemu.' + target_type + '.' + target_name,
3926 '@INPUT@', '@OUTPUT@'
3928 depend_files: tracetool_depends)
3934 # Other build targets
3936 if get_option('plugins')
3937 install_headers('include/qemu/qemu-plugin.h')
3942 # Don't build qemu-keymap if xkbcommon is not explicitly enabled
3943 # when we don't build tools or system
3944 if xkbcommon.found()
3945 # used for the update-keymaps target, so include rules even if !have_tools
3946 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh,
3947 dependencies: [qemuutil, xkbcommon], install: have_tools)
3951 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep],
3952 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true)
3953 qemu_io = executable('qemu-io', files('qemu-io.c'),
3954 dependencies: [block, qemuutil], install: true)
3955 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'),
3956 dependencies: [blockdev, qemuutil, gnutls, selinux],
3959 subdir('storage-daemon')
3960 subdir('contrib/rdmacm-mux')
3961 subdir('contrib/elf2dmp')
3963 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'),
3964 dependencies: qemuutil,
3968 subdir('contrib/vhost-user-blk')
3969 subdir('contrib/vhost-user-gpu')
3970 subdir('contrib/vhost-user-input')
3971 subdir('contrib/vhost-user-scsi')
3974 if targetos == 'linux'
3975 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'),
3976 dependencies: [qemuutil, libcap_ng],
3978 install_dir: get_option('libexecdir'))
3980 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'),
3981 dependencies: [authz, crypto, io, qom, qemuutil,
3982 libcap_ng, mpathpersist],
3987 subdir('contrib/ivshmem-client')
3988 subdir('contrib/ivshmem-server')
4001 if host_machine.system() == 'windows'
4003 find_program('scripts/nsis.py'),
4005 get_option('prefix'),
4006 meson.current_source_dir(),
4007 glib_pc.get_variable('bindir'),
4010 '-DDISPLAYVERSION=' + meson.project_version(),
4013 nsis_cmd += '-DCONFIG_DOCUMENTATION=y'
4016 nsis_cmd += '-DCONFIG_GTK=y'
4019 nsis = custom_target('nsis',
4020 output: 'qemu-setup-' + meson.project_version() + '.exe',
4021 input: files('qemu.nsi'),
4022 build_always_stale: true,
4023 command: nsis_cmd + ['@INPUT@'])
4024 alias_target('installer', nsis)
4027 #########################
4028 # Configuration summary #
4029 #########################
4033 summary_info += {'Build directory': meson.current_build_dir()}
4034 summary_info += {'Source path': meson.current_source_dir()}
4035 summary_info += {'Download dependencies': get_option('wrap_mode') != 'nodownload'}
4036 summary(summary_info, bool_yn: true, section: 'Build environment')
4039 summary_info += {'Install prefix': get_option('prefix')}
4040 summary_info += {'BIOS directory': qemu_datadir}
4041 pathsep = targetos == 'windows' ? ';' : ':'
4042 summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))}
4043 summary_info += {'binary directory': get_option('prefix') / get_option('bindir')}
4044 summary_info += {'library directory': get_option('prefix') / get_option('libdir')}
4045 summary_info += {'module directory': qemu_moddir}
4046 summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')}
4047 summary_info += {'include directory': get_option('prefix') / get_option('includedir')}
4048 summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')}
4049 if targetos != 'windows'
4050 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')}
4051 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')}
4053 summary_info += {'local state directory': 'queried at runtime'}
4055 summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')}
4056 summary(summary_info, bool_yn: true, section: 'Directories')
4060 summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())}
4061 summary_info += {'sphinx-build': sphinx_build}
4063 # FIXME: the [binaries] section of machine files, which can be probed
4064 # with find_program(), would be great for passing gdb and genisoimage
4065 # paths from configure to Meson. However, there seems to be no way to
4066 # hide a program (for example if gdb is too old).
4067 if config_host.has_key('GDB')
4068 summary_info += {'gdb': config_host['GDB']}
4070 summary_info += {'iasl': iasl}
4071 summary_info += {'genisoimage': config_host['GENISOIMAGE']}
4072 if targetos == 'windows' and have_ga
4073 summary_info += {'wixl': wixl}
4075 if slirp.found() and have_system
4076 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false}
4078 summary(summary_info, bool_yn: true, section: 'Host binaries')
4080 # Configurable features
4082 summary_info += {'Documentation': build_docs}
4083 summary_info += {'system-mode emulation': have_system}
4084 summary_info += {'user-mode emulation': have_user}
4085 summary_info += {'block layer': have_block}
4086 summary_info += {'Install blobs': get_option('install_blobs')}
4087 summary_info += {'module support': enable_modules}
4089 summary_info += {'alternative module path': get_option('module_upgrades')}
4091 summary_info += {'fuzzing support': get_option('fuzzing')}
4093 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)}
4095 summary_info += {'Trace backends': ','.join(get_option('trace_backends'))}
4096 if 'simple' in get_option('trace_backends')
4097 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'}
4099 summary_info += {'D-Bus display': dbus_display}
4100 summary_info += {'QOM debugging': get_option('qom_cast_debug')}
4101 summary_info += {'Relocatable install': get_option('relocatable')}
4102 summary_info += {'vhost-kernel support': have_vhost_kernel}
4103 summary_info += {'vhost-net support': have_vhost_net}
4104 summary_info += {'vhost-user support': have_vhost_user}
4105 summary_info += {'vhost-user-crypto support': have_vhost_user_crypto}
4106 summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server}
4107 summary_info += {'vhost-vdpa support': have_vhost_vdpa}
4108 summary_info += {'build guest agent': have_ga}
4109 summary(summary_info, bool_yn: true, section: 'Configurable features')
4111 # Compilation information
4113 summary_info += {'host CPU': cpu}
4114 summary_info += {'host endianness': build_machine.endian()}
4115 summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())}
4116 summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())}
4117 if 'cpp' in all_languages
4118 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())}
4120 summary_info += {'C++ compiler': false}
4122 if 'objc' in all_languages
4123 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())}
4125 summary_info += {'Objective-C compiler': false}
4127 option_cflags = (get_option('debug') ? ['-g'] : [])
4128 if get_option('optimization') != 'plain'
4129 option_cflags += ['-O' + get_option('optimization')]
4131 summary_info += {'CFLAGS': ' '.join(get_option('c_args') + option_cflags)}
4132 if 'cpp' in all_languages
4133 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args') + option_cflags)}
4135 if 'objc' in all_languages
4136 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args') + option_cflags)}
4138 link_args = get_option('c_link_args')
4139 if link_args.length() > 0
4140 summary_info += {'LDFLAGS': ' '.join(link_args)}
4142 summary_info += {'QEMU_CFLAGS': ' '.join(qemu_common_flags + qemu_cflags)}
4143 if 'cpp' in all_languages
4144 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_common_flags + qemu_cxxflags)}
4146 if 'objc' in all_languages
4147 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_common_flags)}
4149 summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)}
4150 summary_info += {'link-time optimization (LTO)': get_option('b_lto')}
4151 summary_info += {'PIE': get_option('b_pie')}
4152 summary_info += {'static build': get_option('prefer_static')}
4153 summary_info += {'malloc trim support': has_malloc_trim}
4154 summary_info += {'membarrier': have_membarrier}
4155 summary_info += {'debug graph lock': get_option('debug_graph_lock')}
4156 summary_info += {'debug stack usage': get_option('debug_stack_usage')}
4157 summary_info += {'mutex debugging': get_option('debug_mutex')}
4158 summary_info += {'memory allocator': get_option('malloc')}
4159 summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')}
4160 summary_info += {'avx512bw optimization': config_host_data.get('CONFIG_AVX512BW_OPT')}
4161 summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')}
4162 summary_info += {'gcov': get_option('b_coverage')}
4163 summary_info += {'thread sanitizer': get_option('tsan')}
4164 summary_info += {'CFI support': get_option('cfi')}
4165 if get_option('cfi')
4166 summary_info += {'CFI debug support': get_option('cfi_debug')}
4168 summary_info += {'strip binaries': get_option('strip')}
4169 summary_info += {'sparse': sparse}
4170 summary_info += {'mingw32 support': targetos == 'windows'}
4171 summary(summary_info, bool_yn: true, section: 'Compilation')
4173 # snarf the cross-compilation information for tests
4176 foreach target: target_dirs
4177 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak'
4178 if fs.exists(tcg_mak)
4179 config_cross_tcg = keyval.load(tcg_mak)
4180 if 'CC' in config_cross_tcg
4181 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']}
4187 summary(summary_info, bool_yn: true, section: 'Cross compilers')
4190 # Targets and accelerators
4193 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')}
4194 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')}
4195 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')}
4196 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')}
4197 summary_info += {'Xen support': xen.found()}
4199 summary_info += {'xen ctrl version': xen.version()}
4201 summary_info += {'Xen emulation': config_all.has_key('CONFIG_XEN_EMU')}
4203 summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')}
4204 if config_all.has_key('CONFIG_TCG')
4205 if get_option('tcg_interpreter')
4206 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'}
4208 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)}
4210 summary_info += {'TCG plugins': get_option('plugins')}
4211 summary_info += {'TCG debug enabled': get_option('debug_tcg')}
4213 summary_info += {'target list': ' '.join(target_dirs)}
4215 summary_info += {'default devices': get_option('default_devices')}
4216 summary_info += {'out of process emulation': multiprocess_allowed}
4217 summary_info += {'vfio-user server': vfio_user_server_allowed}
4219 summary(summary_info, bool_yn: true, section: 'Targets and accelerators')
4223 summary_info += {'coroutine backend': coroutine_backend}
4224 summary_info += {'coroutine pool': have_coroutine_pool}
4226 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')}
4227 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')}
4228 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')}
4229 summary_info += {'VirtFS (9P) support': have_virtfs}
4230 summary_info += {'VirtFS (9P) Proxy Helper support (deprecated)': have_virtfs_proxy_helper}
4231 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')}
4232 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')}
4233 summary_info += {'bochs support': get_option('bochs').allowed()}
4234 summary_info += {'cloop support': get_option('cloop').allowed()}
4235 summary_info += {'dmg support': get_option('dmg').allowed()}
4236 summary_info += {'qcow v1 support': get_option('qcow1').allowed()}
4237 summary_info += {'vdi support': get_option('vdi').allowed()}
4238 summary_info += {'vhdx support': get_option('vhdx').allowed()}
4239 summary_info += {'vmdk support': get_option('vmdk').allowed()}
4240 summary_info += {'vpc support': get_option('vpc').allowed()}
4241 summary_info += {'vvfat support': get_option('vvfat').allowed()}
4242 summary_info += {'qed support': get_option('qed').allowed()}
4243 summary_info += {'parallels support': get_option('parallels').allowed()}
4244 summary_info += {'FUSE exports': fuse}
4245 summary_info += {'VDUSE block exports': have_vduse_blk_export}
4247 summary(summary_info, bool_yn: true, section: 'Block layer support')
4251 summary_info += {'TLS priority': get_option('tls_priority')}
4252 summary_info += {'GNUTLS support': gnutls}
4254 summary_info += {' GNUTLS crypto': gnutls_crypto.found()}
4256 summary_info += {'libgcrypt': gcrypt}
4257 summary_info += {'nettle': nettle}
4259 summary_info += {' XTS': xts != 'private'}
4261 summary_info += {'AF_ALG support': have_afalg}
4262 summary_info += {'rng-none': get_option('rng_none')}
4263 summary_info += {'Linux keyring': have_keyring}
4264 summary_info += {'Linux keyutils': keyutils}
4265 summary(summary_info, bool_yn: true, section: 'Crypto')
4269 if targetos == 'darwin'
4270 summary_info += {'Cocoa support': cocoa}
4272 summary_info += {'SDL support': sdl}
4273 summary_info += {'SDL image support': sdl_image}
4274 summary_info += {'GTK support': gtk}
4275 summary_info += {'pixman': pixman}
4276 summary_info += {'VTE support': vte}
4277 summary_info += {'PNG support': png}
4278 summary_info += {'VNC support': vnc}
4280 summary_info += {'VNC SASL support': sasl}
4281 summary_info += {'VNC JPEG support': jpeg}
4283 summary_info += {'spice protocol support': spice_protocol}
4284 if spice_protocol.found()
4285 summary_info += {' spice server support': spice}
4287 summary_info += {'curses support': curses}
4288 summary_info += {'brlapi support': brlapi}
4289 summary(summary_info, bool_yn: true, section: 'User interface')
4293 if targetos not in ['darwin', 'haiku', 'windows']
4294 summary_info += {'OSS support': oss}
4295 summary_info += {'sndio support': sndio}
4296 elif targetos == 'darwin'
4297 summary_info += {'CoreAudio support': coreaudio}
4298 elif targetos == 'windows'
4299 summary_info += {'DirectSound support': dsound}
4301 if targetos == 'linux'
4302 summary_info += {'ALSA support': alsa}
4303 summary_info += {'PulseAudio support': pulse}
4305 summary_info += {'PipeWire support': pipewire}
4306 summary_info += {'JACK support': jack}
4307 summary(summary_info, bool_yn: true, section: 'Audio backends')
4311 if targetos == 'darwin'
4312 summary_info += {'vmnet.framework support': vmnet}
4314 summary_info += {'AF_XDP support': libxdp}
4315 summary_info += {'slirp support': slirp}
4316 summary_info += {'vde support': vde}
4317 summary_info += {'netmap support': have_netmap}
4318 summary_info += {'l2tpv3 support': have_l2tpv3}
4319 summary(summary_info, bool_yn: true, section: 'Network backends')
4323 summary_info += {'libtasn1': tasn1}
4324 summary_info += {'PAM': pam}
4325 summary_info += {'iconv support': iconv}
4326 summary_info += {'virgl support': virgl}
4327 summary_info += {'rutabaga support': rutabaga}
4328 summary_info += {'blkio support': blkio}
4329 summary_info += {'curl support': curl}
4330 summary_info += {'Multipath support': mpathpersist}
4331 summary_info += {'Linux AIO support': libaio}
4332 summary_info += {'Linux io_uring support': linux_io_uring}
4333 summary_info += {'ATTR/XATTR support': libattr}
4334 summary_info += {'RDMA support': rdma}
4335 summary_info += {'PVRDMA support': have_pvrdma}
4336 summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt}
4337 summary_info += {'libcap-ng support': libcap_ng}
4338 summary_info += {'bpf support': libbpf}
4339 summary_info += {'rbd support': rbd}
4340 summary_info += {'smartcard support': cacard}
4341 summary_info += {'U2F support': u2f}
4342 summary_info += {'libusb': libusb}
4343 summary_info += {'usb net redir': usbredir}
4344 summary_info += {'OpenGL support (epoxy)': opengl}
4345 summary_info += {'GBM': gbm}
4346 summary_info += {'libiscsi support': libiscsi}
4347 summary_info += {'libnfs support': libnfs}
4348 if targetos == 'windows'
4350 summary_info += {'QGA VSS support': have_qga_vss}
4353 summary_info += {'seccomp support': seccomp}
4354 summary_info += {'GlusterFS support': glusterfs}
4355 summary_info += {'hv-balloon support': hv_balloon}
4356 summary_info += {'TPM support': have_tpm}
4357 summary_info += {'libssh support': libssh}
4358 summary_info += {'lzo support': lzo}
4359 summary_info += {'snappy support': snappy}
4360 summary_info += {'bzip2 support': libbzip2}
4361 summary_info += {'lzfse support': liblzfse}
4362 summary_info += {'zstd support': zstd}
4363 summary_info += {'NUMA host support': numa}
4364 summary_info += {'capstone': capstone}
4365 summary_info += {'libpmem support': libpmem}
4366 summary_info += {'libdaxctl support': libdaxctl}
4367 summary_info += {'libudev': libudev}
4368 # Dummy dependency, keep .found()
4369 summary_info += {'FUSE lseek': fuse_lseek.found()}
4370 summary_info += {'selinux': selinux}
4371 summary_info += {'libdw': libdw}
4372 summary(summary_info, bool_yn: true, section: 'Dependencies')
4374 if host_arch == 'unknown'
4376 warning('UNSUPPORTED HOST CPU')
4378 message('Support for CPU host architecture ' + cpu + ' is not currently')
4379 message('maintained. The QEMU project does not guarantee that QEMU will')
4380 message('compile or work on this host CPU. You can help by volunteering')
4381 message('to maintain it and providing a build host for our continuous')
4382 message('integration setup.')
4383 if get_option('tcg').allowed() and target_dirs.length() > 0
4385 message('configure has succeeded and you can continue to build, but')
4386 message('QEMU will use a slow interpreter to emulate the target CPU.')
4390 if not supported_oses.contains(targetos)
4392 warning('UNSUPPORTED HOST OS')
4394 message('Support for host OS ' + targetos + 'is not currently maintained.')
4395 message('configure has succeeded and you can continue to build, but')
4396 message('the QEMU project does not guarantee that QEMU will compile or')
4397 message('work on this operating system. You can help by volunteering')
4398 message('to maintain it and providing a build host for our continuous')
4399 message('integration setup. This will ensure that future versions of QEMU')
4400 message('will keep working on ' + targetos + '.')
4403 if host_arch == 'unknown' or not supported_oses.contains(targetos)
4405 message('If you want to help supporting QEMU on this platform, please')
4406 message('contact the developers at qemu-devel@nongnu.org.')
4409 actually_reloc = get_option('relocatable')
4410 # check if get_relocated_path() is actually able to relocate paths
4411 if get_option('relocatable') and \
4412 not (get_option('prefix') / get_option('bindir')).startswith(get_option('prefix') / '')
4414 warning('bindir not included within prefix, the installation will not be relocatable.')
4415 actually_reloc = false
4417 if not actually_reloc and (targetos == 'windows' or get_option('relocatable'))
4418 if targetos == 'windows'
4420 warning('Windows installs should usually be relocatable.')
4423 message('QEMU will have to be installed under ' + get_option('prefix') + '.')
4424 message('Use --disable-relocatable to remove this warning.')