1 project('qemu', ['c'], meson_version: '>=0.61.3',
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')
20 enable_modules = 'CONFIG_MODULES' in config_host
21 enable_static = 'CONFIG_STATIC' in config_host
23 # Allow both shared and static libraries unless --enable-static
24 static_kwargs = enable_static ? {'static': true} : {}
26 cc = meson.get_compiler('c')
28 if add_languages('cpp', required: false, native: false)
29 all_languages += ['cpp']
30 cxx = meson.get_compiler('cpp')
32 if targetos == 'darwin' and \
33 add_languages('objc', required: get_option('cocoa'), native: false)
34 all_languages += ['objc']
35 objc = meson.get_compiler('objc')
38 # Temporary directory used for files created while
39 # configure runs. Since it is in the build directory
40 # we can safely blow away any previous version of it
41 # (and we need not jump through hoops to try to delete
42 # it when configure exits.)
43 tmpdir = meson.current_build_dir() / 'meson-private/temp'
45 if get_option('qemu_suffix').startswith('/')
46 error('qemu_suffix cannot start with a /')
49 qemu_confdir = get_option('sysconfdir') / get_option('qemu_suffix')
50 qemu_datadir = get_option('datadir') / get_option('qemu_suffix')
51 qemu_docdir = get_option('docdir') / get_option('qemu_suffix')
52 qemu_moddir = get_option('libdir') / get_option('qemu_suffix')
54 qemu_desktopdir = get_option('datadir') / 'applications'
55 qemu_icondir = get_option('datadir') / 'icons'
57 config_host_data = configuration_data()
59 qapi_trace_events = []
61 bsd_oses = ['gnu/kfreebsd', 'freebsd', 'netbsd', 'openbsd', 'dragonfly', 'darwin']
62 supported_oses = ['windows', 'freebsd', 'netbsd', 'openbsd', 'darwin', 'sunos', 'linux']
63 supported_cpus = ['ppc', 'ppc64', 's390x', 'riscv', 'x86', 'x86_64',
64 'arm', 'aarch64', 'loongarch64', 'mips', 'mips64', 'sparc64']
66 cpu = host_machine.cpu_family()
68 # Unify riscv* to a single family.
69 if cpu in ['riscv32', 'riscv64']
73 target_dirs = config_host['TARGET_DIRS'].split()
74 have_linux_user = false
77 foreach target : target_dirs
78 have_linux_user = have_linux_user or target.endswith('linux-user')
79 have_bsd_user = have_bsd_user or target.endswith('bsd-user')
80 have_system = have_system or target.endswith('-softmmu')
82 have_user = have_linux_user or have_bsd_user
83 have_tools = get_option('tools') \
84 .disable_auto_if(not have_system) \
86 have_ga = get_option('guest_agent') \
87 .disable_auto_if(not have_system and not have_tools) \
88 .require(targetos in ['sunos', 'linux', 'windows', 'freebsd', 'netbsd', 'openbsd'],
89 error_message: 'unsupported OS for QEMU guest agent') \
91 have_block = have_system or have_tools
93 python = import('python').find_installation()
95 if cpu not in supported_cpus
105 if cpu in ['x86', 'x86_64']
106 kvm_targets = ['i386-softmmu', 'x86_64-softmmu']
107 elif cpu == 'aarch64'
108 kvm_targets = ['aarch64-softmmu']
110 kvm_targets = ['s390x-softmmu']
111 elif cpu in ['ppc', 'ppc64']
112 kvm_targets = ['ppc-softmmu', 'ppc64-softmmu']
113 elif cpu in ['mips', 'mips64']
114 kvm_targets = ['mips-softmmu', 'mipsel-softmmu', 'mips64-softmmu', 'mips64el-softmmu']
115 elif cpu in ['riscv']
116 kvm_targets = ['riscv32-softmmu', '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'],
141 if cpu in ['x86', 'x86_64']
142 accelerator_targets += {
143 'CONFIG_HAX': ['i386-softmmu', 'x86_64-softmmu'],
144 'CONFIG_HVF': ['x86_64-softmmu'],
145 'CONFIG_NVMM': ['i386-softmmu', 'x86_64-softmmu'],
146 'CONFIG_WHPX': ['i386-softmmu', 'x86_64-softmmu'],
151 # Darwin does not support references to thread-local variables in modules
152 if targetos != 'darwin'
153 modular_tcg = ['i386-softmmu', 'x86_64-softmmu']
156 edk2_targets = [ 'arm-softmmu', 'aarch64-softmmu', 'i386-softmmu', 'x86_64-softmmu' ]
157 unpack_edk2_blobs = false
158 foreach target : edk2_targets
159 if target in target_dirs
160 bzip2 = find_program('bzip2', required: get_option('install_blobs'))
161 unpack_edk2_blobs = bzip2.found()
168 if 'dtrace' in get_option('trace_backends')
169 dtrace = find_program('dtrace', required: true)
170 stap = find_program('stap', required: false)
172 # Workaround to avoid dtrace(1) producing a file with 'hidden' symbol
173 # visibility. Define STAP_SDT_V2 to produce 'default' symbol visibility
174 # instead. QEMU --enable-modules depends on this because the SystemTap
175 # semaphores are linked into the main binary and not the module's shared
177 add_global_arguments('-DSTAP_SDT_V2',
178 native: false, language: all_languages)
182 if get_option('iasl') == ''
183 iasl = find_program('iasl', required: false)
185 iasl = find_program(get_option('iasl'), required: true)
192 qemu_cflags = config_host['QEMU_CFLAGS'].split()
193 qemu_objcflags = config_host['QEMU_OBJCFLAGS'].split()
194 qemu_ldflags = config_host['QEMU_LDFLAGS'].split()
197 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static'
200 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
201 # The combination is known as "full relro", because .got.plt is read-only too.
202 qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now')
204 if targetos == 'windows'
205 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--no-seh', '-Wl,--nxcompat')
206 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--dynamicbase', '-Wl,--high-entropy-va')
209 if get_option('gprof')
210 qemu_cflags += ['-p']
211 qemu_objcflags += ['-p']
212 qemu_ldflags += ['-p']
215 # Specify linker-script with add_project_link_arguments so that it is not placed
216 # within a linker --start-group/--end-group pair
217 if get_option('fuzzing')
218 add_project_link_arguments(['-Wl,-T,',
219 (meson.current_source_dir() / 'tests/qtest/fuzz/fork_fuzz.ld')],
220 native: false, language: all_languages)
222 # Specify a filter to only instrument code that is directly related to
224 configure_file(output: 'instrumentation-filter',
225 input: 'scripts/oss-fuzz/instrumentation-filter-template',
228 if cc.compiles('int main () { return 0; }',
229 name: '-fsanitize-coverage-allowlist=/dev/null',
230 args: ['-fsanitize-coverage-allowlist=/dev/null',
231 '-fsanitize-coverage=trace-pc'] )
232 add_global_arguments('-fsanitize-coverage-allowlist=instrumentation-filter',
233 native: false, language: all_languages)
236 if get_option('fuzzing_engine') == ''
237 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the
238 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link
239 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be
240 # unable to bind the fuzzer-related callbacks added by instrumentation.
241 add_global_arguments('-fsanitize=fuzzer-no-link',
242 native: false, language: all_languages)
243 add_global_link_arguments('-fsanitize=fuzzer-no-link',
244 native: false, language: all_languages)
245 # For the actual fuzzer binaries, we need to link against the libfuzzer
246 # library. They need to be configurable, to support OSS-Fuzz
247 fuzz_exe_ldflags = ['-fsanitize=fuzzer']
249 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and
250 # the needed CFLAGS have already been provided
251 fuzz_exe_ldflags = get_option('fuzzing_engine').split()
255 # Check that the C++ compiler exists and works with the C compiler.
259 if 'cpp' in all_languages
260 add_global_arguments(['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'],
261 native: false, language: 'cpp')
262 foreach k: qemu_cflags
263 if k not in ['-Wstrict-prototypes', '-Wmissing-prototypes', '-Wnested-externs',
264 '-Wold-style-declaration', '-Wold-style-definition', '-Wredundant-decls']
269 if cxx.links(files('scripts/main.c'), args: qemu_cflags)
270 link_language = 'cpp'
273 message('C++ compiler does not work with C compiler')
274 message('Disabling C++-specific optional code')
278 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
279 if targetos != 'sunos' and not config_host.has_key('CONFIG_TSAN')
280 qemu_ldflags += linker.get_supported_link_arguments('-Wl,--warn-common')
283 add_global_link_arguments(qemu_ldflags, native: false, language: all_languages)
285 add_global_arguments(qemu_cflags, native: false, language: 'c')
286 add_global_arguments(qemu_cxxflags, native: false, language: 'cpp')
287 add_global_arguments(qemu_objcflags, native: false, language: 'objc')
288 if targetos == 'linux'
289 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers',
290 '-isystem', 'linux-headers',
291 language: all_languages)
294 add_project_arguments('-iquote', '.',
295 '-iquote', meson.current_source_dir(),
296 '-iquote', meson.current_source_dir() / 'include',
297 language: all_languages)
299 sparse = find_program('cgcc', required: get_option('sparse'))
302 command: [find_program('scripts/check_sparse.py'),
303 'compile_commands.json', sparse.full_path(), '-Wbitwise',
304 '-Wno-transparent-union', '-Wno-old-initializer',
305 '-Wno-non-pointer-null'])
308 ###########################################
309 # Target-specific checks and dependencies #
310 ###########################################
313 if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \
316 #include <sys/types.h>
317 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
318 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
320 args: ['-Werror', '-fsanitize=fuzzer'])
321 error('Your compiler does not support -fsanitize=fuzzer')
325 if 'ftrace' in get_option('trace_backends') and targetos != 'linux'
326 error('ftrace is supported only on Linux')
328 if 'syslog' in get_option('trace_backends') and not cc.compiles('''
331 openlog("qemu", LOG_PID, LOG_DAEMON);
332 syslog(LOG_INFO, "configure");
335 error('syslog is not supported on this system')
338 # Miscellaneous Linux-only features
339 get_option('mpath') \
340 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux')
342 multiprocess_allowed = get_option('multiprocess') \
343 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \
346 vfio_user_server_allowed = get_option('vfio_user_server') \
347 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \
350 have_tpm = get_option('tpm') \
351 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \
355 have_vhost_user = get_option('vhost_user') \
356 .disable_auto_if(targetos != 'linux') \
357 .require(targetos != 'windows',
358 error_message: 'vhost-user is not available on Windows').allowed()
359 have_vhost_vdpa = get_option('vhost_vdpa') \
360 .require(targetos == 'linux',
361 error_message: 'vhost-vdpa is only available on Linux').allowed()
362 have_vhost_kernel = get_option('vhost_kernel') \
363 .require(targetos == 'linux',
364 error_message: 'vhost-kernel is only available on Linux').allowed()
365 have_vhost_user_crypto = get_option('vhost_crypto') \
366 .require(have_vhost_user,
367 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed()
369 have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel
371 have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed()
372 have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed()
373 have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed()
374 have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa
376 # Target-specific libraries and flags
377 libm = cc.find_library('m', required: false)
378 threads = dependency('threads')
379 util = cc.find_library('util', required: false)
385 emulator_link_args = []
392 if targetos == 'windows'
393 midl = find_program('midl', required: false)
394 widl = find_program('widl', required: false)
395 pathcch = cc.find_library('pathcch')
396 socket = cc.find_library('ws2_32')
397 winmm = cc.find_library('winmm')
399 win = import('windows')
400 version_res = win.compile_resources('version.rc',
401 depend_files: files('pc-bios/qemu-nsis.ico'),
402 include_directories: include_directories('.'))
404 elif targetos == 'darwin'
405 coref = dependency('appleframeworks', modules: 'CoreFoundation')
406 iokit = dependency('appleframeworks', modules: 'IOKit', required: false)
407 host_dsosuf = '.dylib'
408 elif targetos == 'sunos'
409 socket = [cc.find_library('socket'),
410 cc.find_library('nsl'),
411 cc.find_library('resolv')]
412 elif targetos == 'haiku'
413 socket = [cc.find_library('posix_error_mapper'),
414 cc.find_library('network'),
415 cc.find_library('bsd')]
416 elif targetos == 'openbsd'
417 if get_option('tcg').allowed() and target_dirs.length() > 0
418 # Disable OpenBSD W^X if available
419 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded')
423 # Target-specific configuration of accelerators
425 if get_option('kvm').allowed() and targetos == 'linux'
426 accelerators += 'CONFIG_KVM'
428 if get_option('whpx').allowed() and targetos == 'windows'
429 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64'
430 error('WHPX requires 64-bit host')
431 elif cc.has_header('WinHvPlatform.h', required: get_option('whpx')) and \
432 cc.has_header('WinHvEmulation.h', required: get_option('whpx'))
433 accelerators += 'CONFIG_WHPX'
436 if get_option('hvf').allowed()
437 hvf = dependency('appleframeworks', modules: 'Hypervisor',
438 required: get_option('hvf'))
440 accelerators += 'CONFIG_HVF'
443 if get_option('hax').allowed()
444 if get_option('hax').enabled() or targetos in ['windows', 'darwin', 'netbsd']
445 accelerators += 'CONFIG_HAX'
448 if targetos == 'netbsd'
449 nvmm = cc.find_library('nvmm', required: get_option('nvmm'))
451 accelerators += 'CONFIG_NVMM'
456 if get_option('tcg').allowed()
457 if host_arch == 'unknown'
458 if get_option('tcg_interpreter')
459 warning('Unsupported CPU @0@, will use TCG with TCI (slow)'.format(cpu))
461 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu))
463 elif get_option('tcg_interpreter')
464 warning('Use of the TCG interpreter is not recommended on this host')
465 warning('architecture. There is a native TCG execution backend available')
466 warning('which provides substantially better performance and reliability.')
467 warning('It is strongly recommended to remove the --enable-tcg-interpreter')
468 warning('configuration option on this architecture to use the native')
471 if get_option('tcg_interpreter')
473 elif host_arch == 'x86_64'
475 elif host_arch == 'ppc64'
478 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch,
479 language: all_languages)
481 accelerators += 'CONFIG_TCG'
482 config_host += { 'CONFIG_TCG': 'y' }
485 if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled()
486 error('KVM not available on this platform')
488 if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled()
489 error('HVF not available on this platform')
491 if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled()
492 error('NVMM not available on this platform')
494 if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled()
495 error('WHPX not available on this platform')
502 # The path to glib.h is added to all compilation commands. This was
503 # grandfathered in from the QEMU Makefiles.
504 add_project_arguments(config_host['GLIB_CFLAGS'].split(),
505 native: false, language: all_languages)
506 glib = declare_dependency(compile_args: config_host['GLIB_CFLAGS'].split(),
507 link_args: config_host['GLIB_LIBS'].split(),
508 version: config_host['GLIB_VERSION'],
510 'bindir': config_host['GLIB_BINDIR'],
512 # override glib dep with the configure results (for subprojects)
513 meson.override_dependency('glib-2.0', glib)
516 gdbus_codegen = not_found
517 gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio'
518 if not get_option('gio').auto() or have_system
519 gio = dependency('gio-2.0', required: get_option('gio'),
520 method: 'pkg-config', kwargs: static_kwargs)
521 if gio.found() and not cc.links('''
525 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
527 }''', dependencies: [glib, gio])
528 if get_option('gio').enabled()
529 error('The installed libgio is broken for static linking')
534 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'),
535 required: get_option('gio'))
536 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'),
537 method: 'pkg-config', kwargs: static_kwargs)
538 gio = declare_dependency(dependencies: [gio, gio_unix],
539 version: gio.version())
542 if gdbus_codegen.found() and get_option('cfi')
543 gdbus_codegen = not_found
544 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity'
548 if 'ust' in get_option('trace_backends')
549 lttng = dependency('lttng-ust', required: true, version: '>= 2.1',
550 method: 'pkg-config', kwargs: static_kwargs)
553 if have_system or have_tools
554 pixman = dependency('pixman-1', required: have_system, version:'>=0.21.8',
555 method: 'pkg-config', kwargs: static_kwargs)
557 zlib = dependency('zlib', required: true, kwargs: static_kwargs)
560 if not get_option('linux_aio').auto() or have_block
561 libaio = cc.find_library('aio', has_headers: ['libaio.h'],
562 required: get_option('linux_aio'),
563 kwargs: static_kwargs)
566 linux_io_uring_test = '''
567 #include <liburing.h>
568 #include <linux/errqueue.h>
570 int main(void) { return 0; }'''
572 linux_io_uring = not_found
573 if not get_option('linux_io_uring').auto() or have_block
574 linux_io_uring = dependency('liburing', version: '>=0.3',
575 required: get_option('linux_io_uring'),
576 method: 'pkg-config', kwargs: static_kwargs)
577 if not cc.links(linux_io_uring_test)
578 linux_io_uring = not_found
583 if not get_option('libnfs').auto() or have_block
584 libnfs = dependency('libnfs', version: '>=1.9.3',
585 required: get_option('libnfs'),
586 method: 'pkg-config', kwargs: static_kwargs)
591 #include <sys/types.h>
592 #ifdef CONFIG_LIBATTR
593 #include <attr/xattr.h>
595 #include <sys/xattr.h>
597 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }'''
600 have_old_libattr = false
601 if get_option('attr').allowed()
602 if cc.links(libattr_test)
603 libattr = declare_dependency()
605 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'],
606 required: get_option('attr'),
607 kwargs: static_kwargs)
608 if libattr.found() and not \
609 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR')
611 if get_option('attr').enabled()
612 error('could not link libattr')
614 warning('could not link libattr, disabling')
617 have_old_libattr = libattr.found()
622 cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'],
623 required: get_option('cocoa'))
625 vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet'))
626 if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h',
627 'VMNET_BRIDGED_MODE',
630 if get_option('vmnet').enabled()
631 error('vmnet.framework API is outdated')
633 warning('vmnet.framework API is outdated, disabling')
638 seccomp_has_sysrawrc = false
639 if not get_option('seccomp').auto() or have_system or have_tools
640 seccomp = dependency('libseccomp', version: '>=2.3.0',
641 required: get_option('seccomp'),
642 method: 'pkg-config', kwargs: static_kwargs)
644 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h',
645 'SCMP_FLTATR_API_SYSRAWRC',
646 dependencies: seccomp)
650 libcap_ng = not_found
651 if not get_option('cap_ng').auto() or have_system or have_tools
652 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'],
653 required: get_option('cap_ng'),
654 kwargs: static_kwargs)
656 if libcap_ng.found() and not cc.links('''
660 capng_capability_to_name(CAPNG_EFFECTIVE);
662 }''', dependencies: libcap_ng)
663 libcap_ng = not_found
664 if get_option('cap_ng').enabled()
665 error('could not link libcap-ng')
667 warning('could not link libcap-ng, disabling')
671 if get_option('xkbcommon').auto() and not have_system and not have_tools
672 xkbcommon = not_found
674 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'),
675 method: 'pkg-config', kwargs: static_kwargs)
679 if not get_option('slirp').auto() or have_system
680 slirp = dependency('slirp', required: get_option('slirp'),
681 method: 'pkg-config', kwargs: static_kwargs)
682 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because
683 # it passes function pointers within libslirp as callbacks for timers.
684 # When using a system-wide shared libslirp, the type information for the
685 # callback is missing and the timer call produces a false positive with CFI.
686 # Do not use the "version" keyword argument to produce a better error.
687 # with control-flow integrity.
688 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7')
689 if get_option('slirp').enabled()
690 error('Control-Flow Integrity requires libslirp 4.7.')
692 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.')
699 if not get_option('vde').auto() or have_system or have_tools
700 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'],
701 required: get_option('vde'),
702 kwargs: static_kwargs)
704 if vde.found() and not cc.links('''
705 #include <libvdeplug.h>
708 struct vde_open_args a = {0, 0, 0};
712 }''', dependencies: vde)
714 if get_option('cap_ng').enabled()
715 error('could not link libvdeplug')
717 warning('could not link libvdeplug, disabling')
722 if not get_option('pa').auto() or (targetos == 'linux' and have_system)
723 pulse = dependency('libpulse', required: get_option('pa'),
724 method: 'pkg-config', kwargs: static_kwargs)
727 if not get_option('alsa').auto() or (targetos == 'linux' and have_system)
728 alsa = dependency('alsa', required: get_option('alsa'),
729 method: 'pkg-config', kwargs: static_kwargs)
732 if not get_option('jack').auto() or have_system
733 jack = dependency('jack', required: get_option('jack'),
734 method: 'pkg-config', kwargs: static_kwargs)
737 if not get_option('sndio').auto() or have_system
738 sndio = dependency('sndio', required: get_option('sndio'),
739 method: 'pkg-config', kwargs: static_kwargs)
742 spice_protocol = not_found
743 if not get_option('spice_protocol').auto() or have_system
744 spice_protocol = dependency('spice-protocol', version: '>=0.12.3',
745 required: get_option('spice_protocol'),
746 method: 'pkg-config', kwargs: static_kwargs)
749 if not get_option('spice').auto() or have_system
750 spice = dependency('spice-server', version: '>=0.12.5',
751 required: get_option('spice'),
752 method: 'pkg-config', kwargs: static_kwargs)
754 spice_headers = spice.partial_dependency(compile_args: true, includes: true)
756 rt = cc.find_library('rt', required: false)
759 if not get_option('libiscsi').auto() or have_block
760 libiscsi = dependency('libiscsi', version: '>=1.9.0',
761 required: get_option('libiscsi'),
762 method: 'pkg-config', kwargs: static_kwargs)
765 if not get_option('zstd').auto() or have_block
766 zstd = dependency('libzstd', version: '>=1.4.0',
767 required: get_option('zstd'),
768 method: 'pkg-config', kwargs: static_kwargs)
772 have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found()
773 if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu
774 virgl = dependency('virglrenderer',
775 method: 'pkg-config',
776 required: get_option('virglrenderer'),
777 kwargs: static_kwargs)
780 if not get_option('blkio').auto() or have_block
781 blkio = dependency('blkio',
782 method: 'pkg-config',
783 required: get_option('blkio'),
784 kwargs: static_kwargs)
787 if not get_option('curl').auto() or have_block
788 curl = dependency('libcurl', version: '>=7.29.0',
789 method: 'pkg-config',
790 required: get_option('curl'),
791 kwargs: static_kwargs)
794 if targetos == 'linux' and (have_system or have_tools)
795 libudev = dependency('libudev',
796 method: 'pkg-config',
797 required: get_option('libudev'),
798 kwargs: static_kwargs)
801 mpathlibs = [libudev]
802 mpathpersist = not_found
803 mpathpersist_new_api = false
804 if targetos == 'linux' and have_tools and get_option('mpath').allowed()
805 mpath_test_source_new = '''
807 #include <mpath_persist.h>
808 unsigned mpath_mx_alloc_len = 1024;
810 static struct config *multipath_conf;
811 extern struct udev *udev;
812 extern struct config *get_multipath_config(void);
813 extern void put_multipath_config(struct config *conf);
815 struct config *get_multipath_config(void) { return multipath_conf; }
816 void put_multipath_config(struct config *conf) { }
819 multipath_conf = mpath_lib_init();
822 mpath_test_source_old = '''
824 #include <mpath_persist.h>
825 unsigned mpath_mx_alloc_len = 1024;
828 struct udev *udev = udev_new();
829 mpath_lib_init(udev);
832 libmpathpersist = cc.find_library('mpathpersist',
833 required: get_option('mpath'),
834 kwargs: static_kwargs)
835 if libmpathpersist.found()
836 mpathlibs += libmpathpersist
838 mpathlibs += cc.find_library('devmapper',
839 required: get_option('mpath'),
840 kwargs: static_kwargs)
842 mpathlibs += cc.find_library('multipath',
843 required: get_option('mpath'),
844 kwargs: static_kwargs)
845 foreach lib: mpathlibs
851 if mpathlibs.length() == 0
852 msg = 'Dependencies missing for libmpathpersist'
853 elif cc.links(mpath_test_source_new, dependencies: mpathlibs)
854 mpathpersist = declare_dependency(dependencies: mpathlibs)
855 mpathpersist_new_api = true
856 elif cc.links(mpath_test_source_old, dependencies: mpathlibs)
857 mpathpersist = declare_dependency(dependencies: mpathlibs)
859 msg = 'Cannot detect libmpathpersist API'
861 if not mpathpersist.found()
862 if get_option('mpath').enabled()
865 warning(msg + ', disabling')
873 if have_system and get_option('curses').allowed()
875 #if defined(__APPLE__) || defined(__OpenBSD__)
876 #define _XOPEN_SOURCE_EXTENDED 1
883 setlocale(LC_ALL, "");
885 addwstr(L"wide chars\n");
887 add_wch(WACS_DEGREE);
891 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw']
892 curses = dependency(curses_dep_list,
894 method: 'pkg-config',
895 kwargs: static_kwargs)
896 msg = get_option('curses').enabled() ? 'curses library not found' : ''
897 curses_compile_args = ['-DNCURSES_WIDECHAR=1']
899 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses])
900 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses])
902 msg = 'curses package not usable'
906 if not curses.found()
907 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
908 if targetos != 'windows' and not has_curses_h
909 message('Trying with /usr/include/ncursesw')
910 curses_compile_args += ['-I/usr/include/ncursesw']
911 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
914 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw'])
915 foreach curses_libname : curses_libname_list
916 libcurses = cc.find_library(curses_libname,
918 kwargs: static_kwargs)
920 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses)
921 curses = declare_dependency(compile_args: curses_compile_args,
922 dependencies: [libcurses])
925 msg = 'curses library not usable'
931 if get_option('iconv').allowed()
932 foreach link_args : [ ['-liconv'], [] ]
933 # Programs will be linked with glib and this will bring in libiconv on FreeBSD.
934 # We need to use libiconv if available because mixing libiconv's headers with
935 # the system libc does not work.
936 # However, without adding glib to the dependencies -L/usr/local/lib will not be
937 # included in the command line and libiconv will not be found.
941 iconv_t conv = iconv_open("WCHAR_T", "UCS-2");
942 return conv != (iconv_t) -1;
943 }''', args: config_host['GLIB_CFLAGS'].split() + config_host['GLIB_LIBS'].split() + link_args)
944 iconv = declare_dependency(link_args: link_args, dependencies: glib)
949 if curses.found() and not iconv.found()
950 if get_option('iconv').enabled()
951 error('iconv not available')
953 msg = 'iconv required for curses UI but not available'
956 if not curses.found() and msg != ''
957 if get_option('curses').enabled()
960 warning(msg + ', disabling')
966 if not get_option('brlapi').auto() or have_system
967 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'],
968 required: get_option('brlapi'),
969 kwargs: static_kwargs)
970 if brlapi.found() and not cc.links('''
973 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi)
975 if get_option('brlapi').enabled()
976 error('could not link brlapi')
978 warning('could not link brlapi, disabling')
984 if not get_option('sdl').auto() or have_system
985 sdl = dependency('sdl2', required: get_option('sdl'), kwargs: static_kwargs)
986 sdl_image = not_found
989 # work around 2.0.8 bug
990 sdl = declare_dependency(compile_args: '-Wno-undef',
992 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'),
993 method: 'pkg-config', kwargs: static_kwargs)
995 if get_option('sdl_image').enabled()
996 error('sdl-image required, but SDL was @0@'.format(
997 get_option('sdl').disabled() ? 'disabled' : 'not found'))
999 sdl_image = not_found
1003 if not get_option('rbd').auto() or have_block
1004 librados = cc.find_library('rados', required: get_option('rbd'),
1005 kwargs: static_kwargs)
1006 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'],
1007 required: get_option('rbd'),
1008 kwargs: static_kwargs)
1009 if librados.found() and librbd.found()
1012 #include <rbd/librbd.h>
1015 rados_create(&cluster, NULL);
1016 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0)
1020 }''', dependencies: [librbd, librados])
1021 rbd = declare_dependency(dependencies: [librbd, librados])
1022 elif get_option('rbd').enabled()
1023 error('librbd >= 1.12.0 required')
1025 warning('librbd >= 1.12.0 not found, disabling')
1030 glusterfs = not_found
1031 glusterfs_ftruncate_has_stat = false
1032 glusterfs_iocb_has_stat = false
1033 if not get_option('glusterfs').auto() or have_block
1034 glusterfs = dependency('glusterfs-api', version: '>=3',
1035 required: get_option('glusterfs'),
1036 method: 'pkg-config', kwargs: static_kwargs)
1037 if glusterfs.found()
1038 glusterfs_ftruncate_has_stat = cc.links('''
1039 #include <glusterfs/api/glfs.h>
1044 /* new glfs_ftruncate() passes two additional args */
1045 return glfs_ftruncate(NULL, 0, NULL, NULL);
1047 ''', dependencies: glusterfs)
1048 glusterfs_iocb_has_stat = cc.links('''
1049 #include <glusterfs/api/glfs.h>
1051 /* new glfs_io_cbk() passes two additional glfs_stat structs */
1053 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
1059 glfs_io_cbk iocb = &glusterfs_iocb;
1060 iocb(NULL, 0 , NULL, NULL, NULL);
1063 ''', dependencies: glusterfs)
1068 if not get_option('libssh').auto() or have_block
1069 libssh = dependency('libssh', version: '>=0.8.7',
1070 method: 'pkg-config',
1071 required: get_option('libssh'),
1072 kwargs: static_kwargs)
1075 libbzip2 = not_found
1076 if not get_option('bzip2').auto() or have_block
1077 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'],
1078 required: get_option('bzip2'),
1079 kwargs: static_kwargs)
1080 if libbzip2.found() and not cc.links('''
1082 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2)
1083 libbzip2 = not_found
1084 if get_option('bzip2').enabled()
1085 error('could not link libbzip2')
1087 warning('could not link libbzip2, disabling')
1092 liblzfse = not_found
1093 if not get_option('lzfse').auto() or have_block
1094 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'],
1095 required: get_option('lzfse'),
1096 kwargs: static_kwargs)
1098 if liblzfse.found() and not cc.links('''
1100 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse)
1101 liblzfse = not_found
1102 if get_option('lzfse').enabled()
1103 error('could not link liblzfse')
1105 warning('could not link liblzfse, disabling')
1110 if get_option('oss').allowed() and have_system
1111 if not cc.has_header('sys/soundcard.h')
1113 elif targetos == 'netbsd'
1114 oss = cc.find_library('ossaudio', required: get_option('oss'),
1115 kwargs: static_kwargs)
1117 oss = declare_dependency()
1121 if get_option('oss').enabled()
1122 error('OSS not found')
1127 if not get_option('dsound').auto() or (targetos == 'windows' and have_system)
1128 if cc.has_header('dsound.h')
1129 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid'])
1132 if not dsound.found()
1133 if get_option('dsound').enabled()
1134 error('DirectSound not found')
1139 coreaudio = not_found
1140 if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system)
1141 coreaudio = dependency('appleframeworks', modules: 'CoreAudio',
1142 required: get_option('coreaudio'))
1146 if not get_option('opengl').auto() or have_system or have_vhost_user_gpu
1147 epoxy = dependency('epoxy', method: 'pkg-config',
1148 required: get_option('opengl'), kwargs: static_kwargs)
1149 if cc.has_header('epoxy/egl.h', dependencies: epoxy)
1151 elif get_option('opengl').enabled()
1152 error('epoxy/egl.h not found')
1156 if (have_system or have_tools) and (virgl.found() or opengl.found())
1157 gbm = dependency('gbm', method: 'pkg-config', required: false,
1158 kwargs: static_kwargs)
1160 have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found()
1163 gnutls_crypto = not_found
1164 if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system)
1165 # For general TLS support our min gnutls matches
1166 # that implied by our platform support matrix
1168 # For the crypto backends, we look for a newer
1171 # Version 3.6.8 is needed to get XTS
1172 # Version 3.6.13 is needed to get PBKDF
1173 # Version 3.6.14 is needed to get HW accelerated XTS
1175 # If newer enough gnutls isn't available, we can
1176 # still use a different crypto backend to satisfy
1177 # the platform support requirements
1178 gnutls_crypto = dependency('gnutls', version: '>=3.6.14',
1179 method: 'pkg-config',
1181 kwargs: static_kwargs)
1182 if gnutls_crypto.found()
1183 gnutls = gnutls_crypto
1185 # Our min version if all we need is TLS
1186 gnutls = dependency('gnutls', version: '>=3.5.18',
1187 method: 'pkg-config',
1188 required: get_option('gnutls'),
1189 kwargs: static_kwargs)
1193 # We prefer use of gnutls for crypto, unless the options
1194 # explicitly asked for nettle or gcrypt.
1196 # If gnutls isn't available for crypto, then we'll prefer
1197 # gcrypt over nettle for performance reasons.
1203 if get_option('nettle').enabled() and get_option('gcrypt').enabled()
1204 error('Only one of gcrypt & nettle can be enabled')
1207 # Explicit nettle/gcrypt request, so ignore gnutls for crypto
1208 if get_option('nettle').enabled() or get_option('gcrypt').enabled()
1209 gnutls_crypto = not_found
1212 if not gnutls_crypto.found()
1213 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled()
1214 gcrypt = dependency('libgcrypt', version: '>=1.8',
1215 method: 'config-tool',
1216 required: get_option('gcrypt'),
1217 kwargs: static_kwargs)
1218 # Debian has removed -lgpg-error from libgcrypt-config
1219 # as it "spreads unnecessary dependencies" which in
1220 # turn breaks static builds...
1221 if gcrypt.found() and enable_static
1222 gcrypt = declare_dependency(dependencies: [
1224 cc.find_library('gpg-error', required: true, kwargs: static_kwargs)])
1227 if (not get_option('nettle').auto() or have_system) and not gcrypt.found()
1228 nettle = dependency('nettle', version: '>=3.4',
1229 method: 'pkg-config',
1230 required: get_option('nettle'),
1231 kwargs: static_kwargs)
1232 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle)
1238 gmp = dependency('gmp', required: false, method: 'pkg-config', kwargs: static_kwargs)
1239 if nettle.found() and gmp.found()
1240 hogweed = dependency('hogweed', version: '>=3.4',
1241 method: 'pkg-config',
1242 required: get_option('nettle'),
1243 kwargs: static_kwargs)
1250 have_gtk_clipboard = get_option('gtk_clipboard').enabled()
1252 if not get_option('gtk').auto() or have_system
1253 gtk = dependency('gtk+-3.0', version: '>=3.22.0',
1254 method: 'pkg-config',
1255 required: get_option('gtk'),
1256 kwargs: static_kwargs)
1258 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0',
1259 method: 'pkg-config',
1261 kwargs: static_kwargs)
1262 gtk = declare_dependency(dependencies: [gtk, gtkx11])
1264 if not get_option('vte').auto() or have_system
1265 vte = dependency('vte-2.91',
1266 method: 'pkg-config',
1267 required: get_option('vte'),
1268 kwargs: static_kwargs)
1270 elif have_gtk_clipboard
1271 error('GTK clipboard requested, but GTK not found')
1277 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found(),
1278 kwargs: static_kwargs)
1281 if get_option('png').allowed() and have_system
1282 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'),
1283 method: 'pkg-config', kwargs: static_kwargs)
1288 if get_option('vnc').allowed() and have_system
1289 vnc = declare_dependency() # dummy dependency
1290 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'),
1291 method: 'pkg-config', kwargs: static_kwargs)
1292 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'],
1293 required: get_option('vnc_sasl'),
1294 kwargs: static_kwargs)
1296 sasl = declare_dependency(dependencies: sasl,
1297 compile_args: '-DSTRUCT_IOVEC_DEFINED')
1302 if not get_option('auth_pam').auto() or have_system
1303 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'],
1304 required: get_option('auth_pam'),
1305 kwargs: static_kwargs)
1307 if pam.found() and not cc.links('''
1309 #include <security/pam_appl.h>
1311 const char *service_name = "qemu";
1312 const char *user = "frank";
1313 const struct pam_conv pam_conv = { 0 };
1314 pam_handle_t *pamh = NULL;
1315 pam_start(service_name, user, &pam_conv, &pamh);
1317 }''', dependencies: pam)
1319 if get_option('auth_pam').enabled()
1320 error('could not link libpam')
1322 warning('could not link libpam, disabling')
1327 if not get_option('snappy').auto() or have_system
1328 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'],
1329 required: get_option('snappy'),
1330 kwargs: static_kwargs)
1332 if snappy.found() and not linker.links('''
1333 #include <snappy-c.h>
1334 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy)
1336 if get_option('snappy').enabled()
1337 error('could not link libsnappy')
1339 warning('could not link libsnappy, disabling')
1344 if not get_option('lzo').auto() or have_system
1345 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'],
1346 required: get_option('lzo'),
1347 kwargs: static_kwargs)
1349 if lzo.found() and not cc.links('''
1350 #include <lzo/lzo1x.h>
1351 int main(void) { lzo_version(); return 0; }''', dependencies: lzo)
1353 if get_option('lzo').enabled()
1354 error('could not link liblzo2')
1356 warning('could not link liblzo2, disabling')
1361 if not get_option('numa').auto() or have_system or have_tools
1362 numa = cc.find_library('numa', has_headers: ['numa.h'],
1363 required: get_option('numa'),
1364 kwargs: static_kwargs)
1366 if numa.found() and not cc.links('''
1368 int main(void) { return numa_available(); }
1369 ''', dependencies: numa)
1371 if get_option('numa').enabled()
1372 error('could not link numa')
1374 warning('could not link numa, disabling')
1379 if not get_option('rdma').auto() or have_system
1380 libumad = cc.find_library('ibumad', required: get_option('rdma'))
1381 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'],
1382 required: get_option('rdma'),
1383 kwargs: static_kwargs),
1384 cc.find_library('ibverbs', required: get_option('rdma'),
1385 kwargs: static_kwargs),
1387 rdma = declare_dependency(dependencies: rdma_libs)
1388 foreach lib: rdma_libs
1396 if get_option('xen').enabled() or (get_option('xen').auto() and have_system)
1397 xencontrol = dependency('xencontrol', required: false,
1398 method: 'pkg-config', kwargs: static_kwargs)
1399 if xencontrol.found()
1400 xen_pc = declare_dependency(version: xencontrol.version(),
1403 # disabler: true makes xen_pc.found() return false if any is not found
1404 dependency('xenstore', required: false,
1405 method: 'pkg-config', kwargs: static_kwargs,
1407 dependency('xenforeignmemory', required: false,
1408 method: 'pkg-config', kwargs: static_kwargs,
1410 dependency('xengnttab', required: false,
1411 method: 'pkg-config', kwargs: static_kwargs,
1413 dependency('xenevtchn', required: false,
1414 method: 'pkg-config', kwargs: static_kwargs,
1416 dependency('xendevicemodel', required: false,
1417 method: 'pkg-config', kwargs: static_kwargs,
1419 # optional, no "disabler: true"
1420 dependency('xentoolcore', required: false,
1421 method: 'pkg-config', kwargs: static_kwargs)])
1427 xen_tests = [ '4.11.0', '4.10.0', '4.9.0', '4.8.0', '4.7.1', '4.6.0', '4.5.0', '4.2.0' ]
1429 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1430 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1431 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1432 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1433 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1434 '4.6.0': [ 'xenstore', 'xenctrl' ],
1435 '4.5.0': [ 'xenstore', 'xenctrl' ],
1436 '4.2.0': [ 'xenstore', 'xenctrl' ],
1439 foreach ver: xen_tests
1440 # cache the various library tests to avoid polluting the logs
1442 foreach l: xen_libs[ver]
1443 if l not in xen_deps
1444 xen_deps += { l: cc.find_library(l, required: false) }
1446 xen_test_deps += xen_deps[l]
1449 # Use -D to pick just one of the test programs in scripts/xen-detect.c
1450 xen_version = ver.split('.')
1451 xen_ctrl_version = xen_version[0] + \
1452 ('0' + xen_version[1]).substring(-2) + \
1453 ('0' + xen_version[2]).substring(-2)
1454 if cc.links(files('scripts/xen-detect.c'),
1455 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version,
1456 dependencies: xen_test_deps)
1457 xen = declare_dependency(version: ver, dependencies: xen_test_deps)
1463 accelerators += 'CONFIG_XEN'
1464 elif get_option('xen').enabled()
1465 error('could not compile and link Xen test program')
1468 have_xen_pci_passthrough = get_option('xen_pci_passthrough') \
1469 .require(xen.found(),
1470 error_message: 'Xen PCI passthrough requested but Xen not enabled') \
1471 .require(targetos == 'linux',
1472 error_message: 'Xen PCI passthrough not available on this platform') \
1477 if not get_option('smartcard').auto() or have_system
1478 cacard = dependency('libcacard', required: get_option('smartcard'),
1479 version: '>=2.5.1', method: 'pkg-config',
1480 kwargs: static_kwargs)
1484 u2f = dependency('u2f-emu', required: get_option('u2f'),
1485 method: 'pkg-config',
1486 kwargs: static_kwargs)
1490 canokey = dependency('canokey-qemu', required: get_option('canokey'),
1491 method: 'pkg-config',
1492 kwargs: static_kwargs)
1494 usbredir = not_found
1495 if not get_option('usb_redir').auto() or have_system
1496 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'),
1497 version: '>=0.6', method: 'pkg-config',
1498 kwargs: static_kwargs)
1501 if not get_option('libusb').auto() or have_system
1502 libusb = dependency('libusb-1.0', required: get_option('libusb'),
1503 version: '>=1.0.13', method: 'pkg-config',
1504 kwargs: static_kwargs)
1508 if not get_option('libpmem').auto() or have_system
1509 libpmem = dependency('libpmem', required: get_option('libpmem'),
1510 method: 'pkg-config', kwargs: static_kwargs)
1512 libdaxctl = not_found
1513 if not get_option('libdaxctl').auto() or have_system
1514 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'),
1515 version: '>=57', method: 'pkg-config',
1516 kwargs: static_kwargs)
1520 tasn1 = dependency('libtasn1',
1521 method: 'pkg-config',
1522 kwargs: static_kwargs)
1524 keyutils = dependency('libkeyutils', required: false,
1525 method: 'pkg-config', kwargs: static_kwargs)
1527 has_gettid = cc.has_function('gettid')
1530 selinux = dependency('libselinux',
1531 required: get_option('selinux'),
1532 method: 'pkg-config', kwargs: static_kwargs)
1537 if get_option('malloc') == 'system'
1539 get_option('malloc_trim').allowed() and \
1540 cc.links('''#include <malloc.h>
1541 int main(void) { malloc_trim(0); return 0; }''')
1543 has_malloc_trim = false
1544 malloc = cc.find_library(get_option('malloc'), required: true)
1546 if not has_malloc_trim and get_option('malloc_trim').enabled()
1547 if get_option('malloc') == 'system'
1548 error('malloc_trim not available on this platform.')
1550 error('malloc_trim not available with non-libc memory allocator')
1554 # Check whether the glibc provides statx()
1556 gnu_source_prefix = '''
1561 statx_test = gnu_source_prefix + '''
1562 #include <sys/stat.h>
1564 struct statx statxbuf;
1565 statx(0, "", 0, STATX_BASIC_STATS, &statxbuf);
1569 has_statx = cc.links(statx_test)
1571 # Check whether statx() provides mount ID information
1573 statx_mnt_id_test = gnu_source_prefix + '''
1574 #include <sys/stat.h>
1576 struct statx statxbuf;
1577 statx(0, "", 0, STATX_BASIC_STATS | STATX_MNT_ID, &statxbuf);
1578 return statxbuf.stx_mnt_id;
1581 has_statx_mnt_id = cc.links(statx_mnt_id_test)
1583 have_vhost_user_blk_server = get_option('vhost_user_blk_server') \
1584 .require(targetos == 'linux',
1585 error_message: 'vhost_user_blk_server requires linux') \
1586 .require(have_vhost_user,
1587 error_message: 'vhost_user_blk_server requires vhost-user support') \
1588 .disable_auto_if(not have_tools and not have_system) \
1591 if get_option('fuse').disabled() and get_option('fuse_lseek').enabled()
1592 error('Cannot enable fuse-lseek while fuse is disabled')
1595 fuse = dependency('fuse3', required: get_option('fuse'),
1596 version: '>=3.1', method: 'pkg-config',
1597 kwargs: static_kwargs)
1599 fuse_lseek = not_found
1600 if get_option('fuse_lseek').allowed()
1601 if fuse.version().version_compare('>=3.8')
1603 fuse_lseek = declare_dependency()
1604 elif get_option('fuse_lseek').enabled()
1606 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version())
1608 error('fuse-lseek requires libfuse, which was not found')
1613 have_libvduse = (targetos == 'linux')
1614 if get_option('libvduse').enabled()
1615 if targetos != 'linux'
1616 error('libvduse requires linux')
1618 elif get_option('libvduse').disabled()
1619 have_libvduse = false
1622 have_vduse_blk_export = (have_libvduse and targetos == 'linux')
1623 if get_option('vduse_blk_export').enabled()
1624 if targetos != 'linux'
1625 error('vduse_blk_export requires linux')
1626 elif not have_libvduse
1627 error('vduse_blk_export requires libvduse support')
1629 elif get_option('vduse_blk_export').disabled()
1630 have_vduse_blk_export = false
1634 libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config')
1635 if libbpf.found() and not cc.links('''
1636 #include <bpf/libbpf.h>
1639 bpf_object__destroy_skeleton(NULL);
1641 }''', dependencies: libbpf)
1643 if get_option('bpf').enabled()
1644 error('libbpf skeleton test failed')
1646 warning('libbpf skeleton test failed, disabling')
1654 audio_drivers_selected = []
1656 audio_drivers_available = {
1657 'alsa': alsa.found(),
1658 'coreaudio': coreaudio.found(),
1659 'dsound': dsound.found(),
1660 'jack': jack.found(),
1662 'pa': pulse.found(),
1664 'sndio': sndio.found(),
1666 foreach k, v: audio_drivers_available
1667 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v)
1670 # Default to native drivers first, OSS second, SDL third
1671 audio_drivers_priority = \
1672 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \
1673 (targetos == 'linux' ? [] : [ 'sdl' ])
1674 audio_drivers_default = []
1675 foreach k: audio_drivers_priority
1676 if audio_drivers_available[k]
1677 audio_drivers_default += k
1681 foreach k: get_option('audio_drv_list')
1683 audio_drivers_selected += audio_drivers_default
1684 elif not audio_drivers_available[k]
1685 error('Audio driver "@0@" not available.'.format(k))
1687 audio_drivers_selected += k
1691 config_host_data.set('CONFIG_AUDIO_DRIVERS',
1692 '"' + '", "'.join(audio_drivers_selected) + '", ')
1694 if get_option('cfi')
1696 # Check for dependency on LTO
1697 if not get_option('b_lto')
1698 error('Selected Control-Flow Integrity but LTO is disabled')
1700 if config_host.has_key('CONFIG_MODULES')
1701 error('Selected Control-Flow Integrity is not compatible with modules')
1703 # Check for cfi flags. CFI requires LTO so we can't use
1704 # get_supported_arguments, but need a more complex "compiles" which allows
1706 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall',
1707 args: ['-flto', '-fsanitize=cfi-icall'] )
1708 cfi_flags += '-fsanitize=cfi-icall'
1710 error('-fsanitize=cfi-icall is not supported by the compiler')
1712 if cc.compiles('int main () { return 0; }',
1713 name: '-fsanitize-cfi-icall-generalize-pointers',
1714 args: ['-flto', '-fsanitize=cfi-icall',
1715 '-fsanitize-cfi-icall-generalize-pointers'] )
1716 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers'
1718 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler')
1720 if get_option('cfi_debug')
1721 if cc.compiles('int main () { return 0; }',
1722 name: '-fno-sanitize-trap=cfi-icall',
1723 args: ['-flto', '-fsanitize=cfi-icall',
1724 '-fno-sanitize-trap=cfi-icall'] )
1725 cfi_flags += '-fno-sanitize-trap=cfi-icall'
1727 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler')
1730 add_global_arguments(cfi_flags, native: false, language: all_languages)
1731 add_global_link_arguments(cfi_flags, native: false, language: all_languages)
1734 have_host_block_device = (targetos != 'darwin' or
1735 cc.has_header('IOKit/storage/IOMedia.h'))
1737 dbus_display = get_option('dbus_display') \
1738 .require(gio.version().version_compare('>=2.64'),
1739 error_message: '-display dbus requires glib>=2.64') \
1740 .require(gdbus_codegen.found(),
1741 error_message: gdbus_codegen_error.format('-display dbus')) \
1742 .require(opengl.found() and gbm.found(),
1743 error_message: '-display dbus requires epoxy/egl and gbm') \
1746 have_virtfs = get_option('virtfs') \
1747 .require(targetos == 'linux' or targetos == 'darwin',
1748 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \
1749 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'),
1750 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \
1751 .require(targetos == 'darwin' or (libattr.found() and libcap_ng.found()),
1752 error_message: 'virtio-9p (virtfs) on Linux requires libcap-ng-devel and libattr-devel') \
1753 .disable_auto_if(not have_tools and not have_system) \
1756 have_virtfs_proxy_helper = targetos != 'darwin' and have_virtfs and have_tools
1758 if get_option('block_drv_ro_whitelist') == ''
1759 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '')
1761 config_host_data.set('CONFIG_BDRV_RO_WHITELIST',
1762 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ')
1764 if get_option('block_drv_rw_whitelist') == ''
1765 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '')
1767 config_host_data.set('CONFIG_BDRV_RW_WHITELIST',
1768 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ')
1771 foreach k : get_option('trace_backends')
1772 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true)
1774 config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file'))
1775 config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority'))
1777 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path())
1779 config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir'))
1780 config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix'))
1781 config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir)
1782 config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir)
1783 config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir)
1785 qemu_firmwarepath = ''
1786 foreach k : get_option('qemu_firmwarepath')
1787 qemu_firmwarepath += '"' + get_option('prefix') / k + '", '
1789 config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath)
1791 config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir'))
1792 config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir)
1793 config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir'))
1794 config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir'))
1795 config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir)
1796 config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir'))
1798 if config_host.has_key('CONFIG_MODULES')
1799 config_host_data.set('CONFIG_STAMP', run_command(
1800 meson.current_source_dir() / 'scripts/qemu-stamp.py',
1801 meson.project_version(), get_option('pkgversion'), '--',
1802 meson.current_source_dir() / 'configure',
1803 capture: true, check: true).stdout().strip())
1806 have_slirp_smbd = get_option('slirp_smbd') \
1807 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \
1810 smbd_path = get_option('smbd')
1812 smbd_path = (targetos == 'solaris' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd')
1814 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path)
1817 config_host_data.set('HOST_' + host_arch.to_upper(), 1)
1819 if get_option('module_upgrades') and not enable_modules
1820 error('Cannot enable module-upgrades as modules are not enabled')
1822 config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades'))
1824 config_host_data.set('CONFIG_ATTR', libattr.found())
1825 config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools'))
1826 config_host_data.set('CONFIG_BRLAPI', brlapi.found())
1827 config_host_data.set('CONFIG_COCOA', cocoa.found())
1828 config_host_data.set('CONFIG_FUZZ', get_option('fuzzing'))
1829 config_host_data.set('CONFIG_GCOV', get_option('b_coverage'))
1830 config_host_data.set('CONFIG_LIBUDEV', libudev.found())
1831 config_host_data.set('CONFIG_LZO', lzo.found())
1832 config_host_data.set('CONFIG_MPATH', mpathpersist.found())
1833 config_host_data.set('CONFIG_MPATH_NEW_API', mpathpersist_new_api)
1834 config_host_data.set('CONFIG_BLKIO', blkio.found())
1835 config_host_data.set('CONFIG_CURL', curl.found())
1836 config_host_data.set('CONFIG_CURSES', curses.found())
1837 config_host_data.set('CONFIG_GBM', gbm.found())
1838 config_host_data.set('CONFIG_GIO', gio.found())
1839 config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found())
1840 if glusterfs.found()
1841 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4'))
1842 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5'))
1843 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6'))
1844 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6'))
1845 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat)
1846 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat)
1848 config_host_data.set('CONFIG_GTK', gtk.found())
1849 config_host_data.set('CONFIG_VTE', vte.found())
1850 config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard)
1851 config_host_data.set('CONFIG_LIBATTR', have_old_libattr)
1852 config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found())
1853 config_host_data.set('CONFIG_EBPF', libbpf.found())
1854 config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found())
1855 config_host_data.set('CONFIG_LIBISCSI', libiscsi.found())
1856 config_host_data.set('CONFIG_LIBNFS', libnfs.found())
1857 config_host_data.set('CONFIG_LIBSSH', libssh.found())
1858 config_host_data.set('CONFIG_LINUX_AIO', libaio.found())
1859 config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found())
1860 config_host_data.set('CONFIG_LIBPMEM', libpmem.found())
1861 config_host_data.set('CONFIG_NUMA', numa.found())
1863 config_host_data.set('HAVE_NUMA_HAS_PREFERRED_MANY',
1864 cc.has_function('numa_has_preferred_many',
1865 dependencies: numa))
1867 config_host_data.set('CONFIG_OPENGL', opengl.found())
1868 config_host_data.set('CONFIG_PROFILER', get_option('profiler'))
1869 config_host_data.set('CONFIG_RBD', rbd.found())
1870 config_host_data.set('CONFIG_RDMA', rdma.found())
1871 config_host_data.set('CONFIG_SDL', sdl.found())
1872 config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found())
1873 config_host_data.set('CONFIG_SECCOMP', seccomp.found())
1875 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc)
1877 config_host_data.set('CONFIG_SNAPPY', snappy.found())
1878 config_host_data.set('CONFIG_TPM', have_tpm)
1879 config_host_data.set('CONFIG_USB_LIBUSB', libusb.found())
1880 config_host_data.set('CONFIG_VDE', vde.found())
1881 config_host_data.set('CONFIG_VHOST_NET', have_vhost_net)
1882 config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user)
1883 config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa)
1884 config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel)
1885 config_host_data.set('CONFIG_VHOST_USER', have_vhost_user)
1886 config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto)
1887 config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa)
1888 config_host_data.set('CONFIG_VMNET', vmnet.found())
1889 config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server)
1890 config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export)
1891 config_host_data.set('CONFIG_PNG', png.found())
1892 config_host_data.set('CONFIG_VNC', vnc.found())
1893 config_host_data.set('CONFIG_VNC_JPEG', jpeg.found())
1894 config_host_data.set('CONFIG_VNC_SASL', sasl.found())
1895 config_host_data.set('CONFIG_VIRTFS', have_virtfs)
1896 config_host_data.set('CONFIG_VTE', vte.found())
1897 config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found())
1898 config_host_data.set('CONFIG_KEYUTILS', keyutils.found())
1899 config_host_data.set('CONFIG_GETTID', has_gettid)
1900 config_host_data.set('CONFIG_GNUTLS', gnutls.found())
1901 config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found())
1902 config_host_data.set('CONFIG_TASN1', tasn1.found())
1903 config_host_data.set('CONFIG_GCRYPT', gcrypt.found())
1904 config_host_data.set('CONFIG_NETTLE', nettle.found())
1905 config_host_data.set('CONFIG_HOGWEED', hogweed.found())
1906 config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private')
1907 config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim)
1908 config_host_data.set('CONFIG_STATX', has_statx)
1909 config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id)
1910 config_host_data.set('CONFIG_ZSTD', zstd.found())
1911 config_host_data.set('CONFIG_FUSE', fuse.found())
1912 config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found())
1913 config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found())
1914 if spice_protocol.found()
1915 config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0])
1916 config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1])
1917 config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2])
1919 config_host_data.set('CONFIG_SPICE', spice.found())
1920 config_host_data.set('CONFIG_X11', x11.found())
1921 config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display)
1922 config_host_data.set('CONFIG_CFI', get_option('cfi'))
1923 config_host_data.set('CONFIG_SELINUX', selinux.found())
1924 config_host_data.set('CONFIG_XEN_BACKEND', xen.found())
1926 # protect from xen.version() having less than three components
1927 xen_version = xen.version().split('.') + ['0', '0']
1928 xen_ctrl_version = xen_version[0] + \
1929 ('0' + xen_version[1]).substring(-2) + \
1930 ('0' + xen_version[2]).substring(-2)
1931 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version)
1933 config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version()))
1934 config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0])
1935 config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1])
1936 config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2])
1938 config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf)
1939 config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device)
1941 have_coroutine_pool = get_option('coroutine_pool')
1942 if get_option('debug_stack_usage') and have_coroutine_pool
1943 message('Disabling coroutine pool to measure stack usage')
1944 have_coroutine_pool = false
1946 config_host_data.set10('CONFIG_COROUTINE_POOL', have_coroutine_pool)
1947 config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex'))
1948 config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage'))
1949 config_host_data.set('CONFIG_GPROF', get_option('gprof'))
1950 config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed())
1951 config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug'))
1952 config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed())
1955 config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h'))
1956 config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h'))
1957 config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h'))
1958 config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h'))
1959 config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h'))
1960 config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h'))
1961 config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h'))
1962 config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h'))
1963 config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h'))
1964 if targetos == 'windows'
1965 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h'))
1969 config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range'))
1970 config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4'))
1971 config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime'))
1972 config_host_data.set('CONFIG_DUP3', cc.has_function('dup3'))
1973 config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate'))
1974 config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate'))
1975 # Note that we need to specify prefix: here to avoid incorrectly
1976 # thinking that Windows has posix_memalign()
1977 config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>'))
1978 config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc'))
1979 config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc'))
1980 config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign'))
1981 config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll'))
1982 config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>'))
1983 config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np'))
1984 config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile'))
1985 config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare'))
1986 config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs'))
1987 config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range'))
1988 config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create'))
1989 config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range'))
1990 config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs'))
1991 config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util))
1992 config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul'))
1993 config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>'))
1995 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS',
1996 cc.has_function('rbd_namespace_exists',
1998 prefix: '#include <rbd/librbd.h>'))
2001 config_host_data.set('HAVE_IBV_ADVISE_MR',
2002 cc.has_function('ibv_advise_mr',
2004 prefix: '#include <infiniband/verbs.h>'))
2008 config_host_data.set('CONFIG_BYTESWAP_H',
2009 cc.has_header_symbol('byteswap.h', 'bswap_32'))
2010 config_host_data.set('CONFIG_EPOLL_CREATE1',
2011 cc.has_header_symbol('sys/epoll.h', 'epoll_create1'))
2012 config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE',
2013 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and
2014 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE'))
2015 config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE',
2016 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE'))
2017 config_host_data.set('CONFIG_FIEMAP',
2018 cc.has_header('linux/fiemap.h') and
2019 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP'))
2020 config_host_data.set('CONFIG_GETRANDOM',
2021 cc.has_function('getrandom') and
2022 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK'))
2023 config_host_data.set('CONFIG_INOTIFY',
2024 cc.has_header_symbol('sys/inotify.h', 'inotify_init'))
2025 config_host_data.set('CONFIG_INOTIFY1',
2026 cc.has_header_symbol('sys/inotify.h', 'inotify_init1'))
2027 config_host_data.set('CONFIG_MACHINE_BSWAP_H',
2028 cc.has_header_symbol('machine/bswap.h', 'bswap32',
2029 prefix: '''#include <sys/endian.h>
2030 #include <sys/types.h>'''))
2031 config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK',
2032 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK'))
2033 config_host_data.set('CONFIG_RTNETLINK',
2034 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN'))
2035 config_host_data.set('CONFIG_SYSMACROS',
2036 cc.has_header_symbol('sys/sysmacros.h', 'makedev'))
2037 config_host_data.set('HAVE_OPTRESET',
2038 cc.has_header_symbol('getopt.h', 'optreset'))
2039 config_host_data.set('HAVE_IPPROTO_MPTCP',
2040 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP'))
2041 config_host_data.set('HAVE_SYS_MOUNT_FSCONFIG',
2042 cc.has_header_symbol('sys/mount.h', 'FSCONFIG_SET_FLAG'))
2045 config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID',
2046 cc.has_member('struct sigevent', 'sigev_notify_thread_id',
2047 prefix: '#include <signal.h>'))
2048 config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM',
2049 cc.has_member('struct stat', 'st_atim',
2050 prefix: '#include <sys/stat.h>'))
2053 config_host_data.set('CONFIG_IOVEC',
2054 cc.has_type('struct iovec',
2055 prefix: '#include <sys/uio.h>'))
2056 config_host_data.set('HAVE_UTMPX',
2057 cc.has_type('struct utmpx',
2058 prefix: '#include <utmpx.h>'))
2060 config_host_data.set('CONFIG_EVENTFD', cc.links('''
2061 #include <sys/eventfd.h>
2062 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }'''))
2063 config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + '''
2066 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
2067 return fdatasync(0);
2069 #error Not supported
2073 has_madvise = cc.links(gnu_source_prefix + '''
2074 #include <sys/types.h>
2075 #include <sys/mman.h>
2077 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''')
2078 missing_madvise_proto = false
2080 # Some platforms (illumos and Solaris before Solaris 11) provide madvise()
2081 # but forget to prototype it. In this case, has_madvise will be true (the
2082 # test program links despite a compile warning). To detect the
2083 # missing-prototype case, we try again with a definitely-bogus prototype.
2084 # This will only compile if the system headers don't provide the prototype;
2085 # otherwise the conflicting prototypes will cause a compiler error.
2086 missing_madvise_proto = cc.links(gnu_source_prefix + '''
2087 #include <sys/types.h>
2088 #include <sys/mman.h>
2090 extern int madvise(int);
2091 int main(void) { return madvise(0); }''')
2093 config_host_data.set('CONFIG_MADVISE', has_madvise)
2094 config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto)
2096 config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + '''
2097 #include <sys/mman.h>
2098 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }'''))
2099 config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + '''
2101 #if !defined(AT_EMPTY_PATH)
2102 # error missing definition
2104 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
2106 config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + '''
2107 #include <sys/mman.h>
2109 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }'''))
2111 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + '''
2112 #include <pthread.h>
2114 static void *f(void *p) { return NULL; }
2118 pthread_create(&thread, 0, f, 0);
2119 pthread_setname_np(thread, "QEMU");
2121 }''', dependencies: threads))
2122 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + '''
2123 #include <pthread.h>
2125 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
2129 pthread_create(&thread, 0, f, 0);
2131 }''', dependencies: threads))
2132 config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + '''
2133 #include <pthread.h>
2138 pthread_condattr_t attr
2139 pthread_condattr_init(&attr);
2140 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC);
2142 }''', dependencies: threads))
2143 config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + '''
2144 #include <pthread.h>
2146 static void *f(void *p) { return NULL; }
2149 int setsize = CPU_ALLOC_SIZE(64);
2152 pthread_create(&thread, 0, f, 0);
2153 cpuset = CPU_ALLOC(64);
2154 CPU_ZERO_S(setsize, cpuset);
2155 pthread_setaffinity_np(thread, setsize, cpuset);
2156 pthread_getaffinity_np(thread, setsize, cpuset);
2159 }''', dependencies: threads))
2160 config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + '''
2161 #include <sys/signalfd.h>
2163 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }'''))
2164 config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + '''
2172 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
2173 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
2177 config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + '''
2178 #include <sys/mman.h>
2180 return mlockall(MCL_FUTURE);
2184 if get_option('l2tpv3').allowed() and have_system
2185 have_l2tpv3 = cc.has_type('struct mmsghdr',
2186 prefix: gnu_source_prefix + '''
2187 #include <sys/socket.h>
2188 #include <linux/ip.h>''')
2190 config_host_data.set('CONFIG_L2TPV3', have_l2tpv3)
2193 if get_option('netmap').allowed() and have_system
2194 have_netmap = cc.compiles('''
2195 #include <inttypes.h>
2197 #include <net/netmap.h>
2198 #include <net/netmap_user.h>
2199 #if (NETMAP_API < 11) || (NETMAP_API > 15)
2202 int main(void) { return 0; }''')
2203 if not have_netmap and get_option('netmap').enabled()
2204 error('Netmap headers not available')
2207 config_host_data.set('CONFIG_NETMAP', have_netmap)
2209 # Work around a system header bug with some kernel/XFS header
2210 # versions where they both try to define 'struct fsxattr':
2211 # xfs headers will not try to redefine structs from linux headers
2212 # if this macro is set.
2213 config_host_data.set('HAVE_FSXATTR', cc.links('''
2214 #include <linux/fs.h>
2220 # Some versions of Mac OS X incorrectly define SIZE_MAX
2221 config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles('''
2225 return printf("%zu", SIZE_MAX);
2226 }''', args: ['-Werror']))
2233 y = __atomic_load_n(&x, __ATOMIC_RELAXED);
2234 __atomic_store_n(&x, y, __ATOMIC_RELAXED);
2235 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2236 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
2237 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
2241 # See if 64-bit atomic operations are supported.
2242 # Note that without __atomic builtins, we can only
2243 # assume atomic loads/stores max at pointer size.
2244 config_host_data.set('CONFIG_ATOMIC64', cc.links(atomic_test.format('uint64_t')))
2246 has_int128 = cc.links('''
2256 config_host_data.set('CONFIG_INT128', has_int128)
2259 # "do we have 128-bit atomics which are handled inline and specifically not
2260 # via libatomic". The reason we can't use libatomic is documented in the
2261 # comment starting "GCC is a house divided" in include/qemu/atomic128.h.
2262 has_atomic128 = cc.links(atomic_test.format('unsigned __int128'))
2264 config_host_data.set('CONFIG_ATOMIC128', has_atomic128)
2266 if not has_atomic128
2267 has_cmpxchg128 = cc.links('''
2270 unsigned __int128 x = 0, y = 0;
2271 __sync_val_compare_and_swap_16(&x, y, x);
2276 config_host_data.set('CONFIG_CMPXCHG128', has_cmpxchg128)
2280 config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + '''
2281 #include <sys/auxv.h>
2283 return getauxval(AT_HWCAP) == 0;
2286 config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles('''
2287 #include <linux/usbdevice_fs.h>
2289 #ifndef USBDEVFS_GET_CAPABILITIES
2290 #error "USBDEVFS_GET_CAPABILITIES undefined"
2293 #ifndef USBDEVFS_DISCONNECT_CLAIM
2294 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
2297 int main(void) { return 0; }'''))
2299 have_keyring = get_option('keyring') \
2300 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \
2301 .require(cc.compiles('''
2303 #include <asm/unistd.h>
2304 #include <linux/keyctl.h>
2305 #include <sys/syscall.h>
2308 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
2309 }'''), error_message: 'keyctl syscall not available on this system').allowed()
2310 config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring)
2312 have_cpuid_h = cc.links('''
2315 unsigned a, b, c, d;
2316 unsigned max = __get_cpuid_max(0, 0);
2319 __cpuid(1, a, b, c, d);
2323 __cpuid_count(7, 0, a, b, c, d);
2328 config_host_data.set('CONFIG_CPUID_H', have_cpuid_h)
2330 config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \
2331 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \
2332 .require(cc.links('''
2333 #pragma GCC push_options
2334 #pragma GCC target("avx2")
2336 #include <immintrin.h>
2337 static int bar(void *a) {
2338 __m256i x = *(__m256i *)a;
2339 return _mm256_testz_si256(x, x);
2341 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2342 '''), error_message: 'AVX2 not available').allowed())
2344 config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \
2345 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \
2346 .require(cc.links('''
2347 #pragma GCC push_options
2348 #pragma GCC target("avx512f")
2350 #include <immintrin.h>
2351 static int bar(void *a) {
2352 __m512i x = *(__m512i *)a;
2353 return _mm512_test_epi64_mask(x, x);
2355 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2356 '''), error_message: 'AVX512F not available').allowed())
2358 have_pvrdma = get_option('pvrdma') \
2359 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \
2360 .require(cc.compiles(gnu_source_prefix + '''
2361 #include <sys/mman.h>
2366 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
2369 }'''), error_message: 'PVRDMA requires mremap').allowed()
2372 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links('''
2373 #include <infiniband/verbs.h>
2377 struct ibv_pd *pd = NULL;
2383 mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
2389 if get_option('membarrier').disabled()
2390 have_membarrier = false
2391 elif targetos == 'windows'
2392 have_membarrier = true
2393 elif targetos == 'linux'
2394 have_membarrier = cc.compiles('''
2395 #include <linux/membarrier.h>
2396 #include <sys/syscall.h>
2400 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
2401 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
2405 config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \
2406 .require(have_membarrier, error_message: 'membarrier system call not available') \
2409 have_afalg = get_option('crypto_afalg') \
2410 .require(cc.compiles(gnu_source_prefix + '''
2412 #include <sys/types.h>
2413 #include <sys/socket.h>
2414 #include <linux/if_alg.h>
2417 sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
2420 '''), error_message: 'AF_ALG requested but could not be detected').allowed()
2421 config_host_data.set('CONFIG_AF_ALG', have_afalg)
2423 config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol(
2424 'linux/vm_sockets.h', 'AF_VSOCK',
2425 prefix: '#include <sys/socket.h>',
2429 have_vss_sdk = false # old xp/2003 SDK
2430 if targetos == 'windows' and link_language == 'cpp'
2431 have_vss = cxx.compiles('''
2432 #define __MIDL_user_allocate_free_DEFINED__
2434 int main(void) { return VSS_CTX_BACKUP; }''')
2435 have_vss_sdk = cxx.has_header('vscoordint.h')
2437 config_host_data.set('HAVE_VSS_SDK', have_vss_sdk)
2439 foreach k, v: config_host
2440 if k.startswith('CONFIG_')
2441 config_host_data.set(k, v == 'y' ? 1 : v)
2445 # Older versions of MinGW do not import _lock_file and _unlock_file properly.
2446 # This was fixed for v6.0.0 with commit b48e3ac8969d.
2447 if targetos == 'windows'
2448 config_host_data.set('HAVE__LOCK_FILE', cc.links('''
2454 }''', name: '_lock_file and _unlock_file'))
2457 ########################
2458 # Target configuration #
2459 ########################
2461 minikconf = find_program('scripts/minikconf.py')
2463 config_all_devices = {}
2464 config_all_disas = {}
2465 config_devices_mak_list = []
2466 config_devices_h = {}
2467 config_target_h = {}
2468 config_target_mak = {}
2471 'alpha' : ['CONFIG_ALPHA_DIS'],
2472 'avr' : ['CONFIG_AVR_DIS'],
2473 'cris' : ['CONFIG_CRIS_DIS'],
2474 'hexagon' : ['CONFIG_HEXAGON_DIS'],
2475 'hppa' : ['CONFIG_HPPA_DIS'],
2476 'i386' : ['CONFIG_I386_DIS'],
2477 'x86_64' : ['CONFIG_I386_DIS'],
2478 'm68k' : ['CONFIG_M68K_DIS'],
2479 'microblaze' : ['CONFIG_MICROBLAZE_DIS'],
2480 'mips' : ['CONFIG_MIPS_DIS'],
2481 'nios2' : ['CONFIG_NIOS2_DIS'],
2482 'or1k' : ['CONFIG_OPENRISC_DIS'],
2483 'ppc' : ['CONFIG_PPC_DIS'],
2484 'riscv' : ['CONFIG_RISCV_DIS'],
2485 'rx' : ['CONFIG_RX_DIS'],
2486 's390' : ['CONFIG_S390_DIS'],
2487 'sh4' : ['CONFIG_SH4_DIS'],
2488 'sparc' : ['CONFIG_SPARC_DIS'],
2489 'xtensa' : ['CONFIG_XTENSA_DIS'],
2490 'loongarch' : ['CONFIG_LOONGARCH_DIS'],
2492 if link_language == 'cpp'
2494 'mips' : [ 'CONFIG_MIPS_DIS', 'CONFIG_NANOMIPS_DIS'],
2498 have_ivshmem = config_host_data.get('CONFIG_EVENTFD')
2500 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \
2501 (have_tpm ? ['CONFIG_TPM=y'] : []) + \
2502 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \
2503 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \
2504 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \
2505 (x11.found() ? ['CONFIG_X11=y'] : []) + \
2506 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \
2507 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \
2508 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \
2509 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \
2510 ('CONFIG_LINUX' in config_host ? ['CONFIG_LINUX=y'] : []) + \
2511 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \
2512 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \
2513 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : [])
2515 ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ]
2517 default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host
2518 actual_target_dirs = []
2520 foreach target : target_dirs
2521 config_target = { 'TARGET_NAME': target.split('-')[0] }
2522 if target.endswith('linux-user')
2523 if targetos != 'linux'
2527 error('Target @0@ is only available on a Linux host'.format(target))
2529 config_target += { 'CONFIG_LINUX_USER': 'y' }
2530 elif target.endswith('bsd-user')
2531 if 'CONFIG_BSD' not in config_host
2535 error('Target @0@ is only available on a BSD host'.format(target))
2537 config_target += { 'CONFIG_BSD_USER': 'y' }
2538 elif target.endswith('softmmu')
2539 config_target += { 'CONFIG_SOFTMMU': 'y' }
2541 if target.endswith('-user')
2543 'CONFIG_USER_ONLY': 'y',
2544 'CONFIG_QEMU_INTERP_PREFIX':
2545 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME'])
2550 foreach sym: accelerators
2551 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, [])
2552 config_target += { sym: 'y' }
2553 config_all += { sym: 'y' }
2554 if sym == 'CONFIG_TCG' and tcg_arch == 'tci'
2555 config_target += { 'CONFIG_TCG_INTERPRETER': 'y' }
2557 if target in modular_tcg
2558 config_target += { 'CONFIG_TCG_MODULAR': 'y' }
2560 config_target += { 'CONFIG_TCG_BUILTIN': 'y' }
2562 accel_kconfig += [ sym + '=y' ]
2565 if accel_kconfig.length() == 0
2569 error('No accelerator available for target @0@'.format(target))
2572 actual_target_dirs += target
2573 config_target += keyval.load('configs/targets' / target + '.mak')
2574 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' }
2576 if 'TARGET_NEED_FDT' in config_target
2577 fdt_required += target
2581 if 'TARGET_BASE_ARCH' not in config_target
2582 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']}
2584 if 'TARGET_ABI_DIR' not in config_target
2585 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']}
2587 if 'TARGET_BIG_ENDIAN' not in config_target
2588 config_target += {'TARGET_BIG_ENDIAN': 'n'}
2591 foreach k, v: disassemblers
2592 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k)
2594 config_target += { sym: 'y' }
2595 config_all_disas += { sym: 'y' }
2600 config_target_data = configuration_data()
2601 foreach k, v: config_target
2602 if not k.startswith('TARGET_') and not k.startswith('CONFIG_')
2604 elif ignored.contains(k)
2606 elif k == 'TARGET_BASE_ARCH'
2607 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is
2608 # not used to select files from sourcesets.
2609 config_target_data.set('TARGET_' + v.to_upper(), 1)
2610 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX'
2611 config_target_data.set_quoted(k, v)
2613 config_target_data.set(k, 1)
2615 config_target_data.set(k, 0)
2617 config_target_data.set(k, v)
2620 config_target_data.set('QEMU_ARCH',
2621 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper())
2622 config_target_h += {target: configure_file(output: target + '-config-target.h',
2623 configuration: config_target_data)}
2625 if target.endswith('-softmmu')
2626 config_input = meson.get_external_property(target, 'default')
2627 config_devices_mak = target + '-config-devices.mak'
2628 config_devices_mak = configure_file(
2629 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'],
2630 output: config_devices_mak,
2631 depfile: config_devices_mak + '.d',
2633 command: [minikconf,
2634 get_option('default_devices') ? '--defconfig' : '--allnoconfig',
2635 config_devices_mak, '@DEPFILE@', '@INPUT@',
2636 host_kconfig, accel_kconfig,
2637 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y'])
2639 config_devices_data = configuration_data()
2640 config_devices = keyval.load(config_devices_mak)
2641 foreach k, v: config_devices
2642 config_devices_data.set(k, 1)
2644 config_devices_mak_list += config_devices_mak
2645 config_devices_h += {target: configure_file(output: target + '-config-devices.h',
2646 configuration: config_devices_data)}
2647 config_target += config_devices
2648 config_all_devices += config_devices
2650 config_target_mak += {target: config_target}
2652 target_dirs = actual_target_dirs
2654 # This configuration is used to build files that are shared by
2655 # multiple binaries, and then extracted out of the "common"
2656 # static_library target.
2658 # We do not use all_sources()/all_dependencies(), because it would
2659 # build literally all source files, including devices only used by
2660 # targets that are not built for this compilation. The CONFIG_ALL
2661 # pseudo symbol replaces it.
2663 config_all += config_all_devices
2664 config_all += config_host
2665 config_all += config_all_disas
2667 'CONFIG_XEN': xen.found(),
2668 'CONFIG_SOFTMMU': have_system,
2669 'CONFIG_USER_ONLY': have_user,
2673 target_configs_h = []
2674 foreach target: target_dirs
2675 target_configs_h += config_target_h[target]
2676 target_configs_h += config_devices_h.get(target, [])
2678 genh += custom_target('config-poison.h',
2679 input: [target_configs_h],
2680 output: 'config-poison.h',
2682 command: [find_program('scripts/make-config-poison.sh'),
2689 capstone = not_found
2690 if not get_option('capstone').auto() or have_system or have_user
2691 capstone = dependency('capstone', version: '>=3.0.5',
2692 kwargs: static_kwargs, method: 'pkg-config',
2693 required: get_option('capstone'))
2695 # Some versions of capstone have broken pkg-config file
2696 # that reports a wrong -I path, causing the #include to
2697 # fail later. If the system has such a broken version
2699 if capstone.found() and not cc.compiles('#include <capstone.h>',
2700 dependencies: [capstone])
2701 capstone = not_found
2702 if get_option('capstone').enabled()
2703 error('capstone requested, but it does not appear to work')
2708 libvfio_user_dep = not_found
2709 if have_system and vfio_user_server_allowed
2710 have_internal = fs.exists(meson.current_source_dir() / 'subprojects/libvfio-user/meson.build')
2712 if not have_internal
2713 error('libvfio-user source not found - please pull git submodule')
2716 libvfio_user_proj = subproject('libvfio-user')
2718 libvfio_user_lib = libvfio_user_proj.get_variable('libvfio_user_dep')
2720 libvfio_user_dep = declare_dependency(dependencies: [libvfio_user_lib])
2725 fdt_opt = get_option('fdt')
2726 if fdt_opt in ['enabled', 'auto', 'system']
2727 have_internal = fs.exists(meson.current_source_dir() / 'dtc/libfdt/Makefile.libfdt')
2728 fdt = cc.find_library('fdt', kwargs: static_kwargs,
2729 required: fdt_opt == 'system' or
2730 fdt_opt == 'enabled' and not have_internal)
2731 if fdt.found() and cc.links('''
2733 #include <libfdt_env.h>
2734 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''',
2737 elif fdt_opt == 'system'
2738 error('system libfdt requested, but it is too old (1.5.1 or newer required)')
2740 fdt_opt = 'internal'
2742 fdt_opt = 'disabled'
2746 if fdt_opt == 'internal'
2749 'dtc/libfdt/fdt_ro.c',
2750 'dtc/libfdt/fdt_wip.c',
2751 'dtc/libfdt/fdt_sw.c',
2752 'dtc/libfdt/fdt_rw.c',
2753 'dtc/libfdt/fdt_strerror.c',
2754 'dtc/libfdt/fdt_empty_tree.c',
2755 'dtc/libfdt/fdt_addresses.c',
2756 'dtc/libfdt/fdt_overlay.c',
2757 'dtc/libfdt/fdt_check.c',
2760 fdt_inc = include_directories('dtc/libfdt')
2761 libfdt = static_library('fdt',
2762 build_by_default: false,
2764 include_directories: fdt_inc)
2765 fdt = declare_dependency(link_with: libfdt,
2766 include_directories: fdt_inc)
2769 fdt_opt = 'disabled'
2771 if not fdt.found() and fdt_required.length() > 0
2772 error('fdt not available but required by targets ' + ', '.join(fdt_required))
2775 config_host_data.set('CONFIG_CAPSTONE', capstone.found())
2776 config_host_data.set('CONFIG_FDT', fdt.found())
2777 config_host_data.set('CONFIG_SLIRP', slirp.found())
2779 #####################
2780 # Generated sources #
2781 #####################
2783 genh += configure_file(output: 'config-host.h', configuration: config_host_data)
2785 hxtool = find_program('scripts/hxtool')
2786 shaderinclude = find_program('scripts/shaderinclude.pl')
2787 qapi_gen = find_program('scripts/qapi-gen.py')
2788 qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py',
2789 meson.current_source_dir() / 'scripts/qapi/commands.py',
2790 meson.current_source_dir() / 'scripts/qapi/common.py',
2791 meson.current_source_dir() / 'scripts/qapi/error.py',
2792 meson.current_source_dir() / 'scripts/qapi/events.py',
2793 meson.current_source_dir() / 'scripts/qapi/expr.py',
2794 meson.current_source_dir() / 'scripts/qapi/gen.py',
2795 meson.current_source_dir() / 'scripts/qapi/introspect.py',
2796 meson.current_source_dir() / 'scripts/qapi/parser.py',
2797 meson.current_source_dir() / 'scripts/qapi/schema.py',
2798 meson.current_source_dir() / 'scripts/qapi/source.py',
2799 meson.current_source_dir() / 'scripts/qapi/types.py',
2800 meson.current_source_dir() / 'scripts/qapi/visit.py',
2801 meson.current_source_dir() / 'scripts/qapi/common.py',
2802 meson.current_source_dir() / 'scripts/qapi-gen.py'
2806 python, files('scripts/tracetool.py'),
2807 '--backend=' + ','.join(get_option('trace_backends'))
2809 tracetool_depends = files(
2810 'scripts/tracetool/backend/log.py',
2811 'scripts/tracetool/backend/__init__.py',
2812 'scripts/tracetool/backend/dtrace.py',
2813 'scripts/tracetool/backend/ftrace.py',
2814 'scripts/tracetool/backend/simple.py',
2815 'scripts/tracetool/backend/syslog.py',
2816 'scripts/tracetool/backend/ust.py',
2817 'scripts/tracetool/format/ust_events_c.py',
2818 'scripts/tracetool/format/ust_events_h.py',
2819 'scripts/tracetool/format/__init__.py',
2820 'scripts/tracetool/format/d.py',
2821 'scripts/tracetool/format/simpletrace_stap.py',
2822 'scripts/tracetool/format/c.py',
2823 'scripts/tracetool/format/h.py',
2824 'scripts/tracetool/format/log_stap.py',
2825 'scripts/tracetool/format/stap.py',
2826 'scripts/tracetool/__init__.py',
2827 'scripts/tracetool/transform.py',
2828 'scripts/tracetool/vcpu.py'
2831 qemu_version_cmd = [find_program('scripts/qemu-version.sh'),
2832 meson.current_source_dir(),
2833 get_option('pkgversion'), meson.project_version()]
2834 qemu_version = custom_target('qemu-version.h',
2835 output: 'qemu-version.h',
2836 command: qemu_version_cmd,
2838 build_by_default: true,
2839 build_always_stale: true)
2840 genh += qemu_version
2844 ['qemu-options.hx', 'qemu-options.def'],
2845 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'],
2849 ['hmp-commands.hx', 'hmp-commands.h'],
2850 ['hmp-commands-info.hx', 'hmp-commands-info.h'],
2853 foreach d : hx_headers
2854 hxdep += custom_target(d[1],
2858 build_by_default: true, # to be removed when added to a target
2859 command: [hxtool, '-h', '@INPUT0@'])
2867 authz_ss = ss.source_set()
2868 blockdev_ss = ss.source_set()
2869 block_ss = ss.source_set()
2870 chardev_ss = ss.source_set()
2871 common_ss = ss.source_set()
2872 crypto_ss = ss.source_set()
2873 hwcore_ss = ss.source_set()
2874 io_ss = ss.source_set()
2875 qmp_ss = ss.source_set()
2876 qom_ss = ss.source_set()
2877 softmmu_ss = ss.source_set()
2878 specific_fuzz_ss = ss.source_set()
2879 specific_ss = ss.source_set()
2880 stub_ss = ss.source_set()
2881 trace_ss = ss.source_set()
2882 user_ss = ss.source_set()
2883 util_ss = ss.source_set()
2886 qtest_module_ss = ss.source_set()
2887 tcg_module_ss = ss.source_set()
2893 target_softmmu_arch = {}
2894 target_user_arch = {}
2900 # TODO: add each directory to the subdirs from its own meson.build, once
2902 trace_events_subdirs = [
2911 trace_events_subdirs += [ 'linux-user' ]
2914 trace_events_subdirs += [ 'bsd-user' ]
2917 trace_events_subdirs += [
2926 trace_events_subdirs += [
2940 'hw/block/dataplane',
2989 if have_system or have_user
2990 trace_events_subdirs += [
3008 vhost_user = not_found
3009 if targetos == 'linux' and have_vhost_user
3010 libvhost_user = subproject('libvhost-user')
3011 vhost_user = libvhost_user.get_variable('vhost_user_dep')
3014 libvduse = not_found
3016 libvduse_proj = subproject('libvduse')
3017 libvduse = libvduse_proj.get_variable('libvduse_dep')
3020 # NOTE: the trace/ subdirectory needs the qapi_trace_events variable
3021 # that is filled in by qapi/.
3036 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO')
3037 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO')
3040 qom_ss = qom_ss.apply(config_host, strict: false)
3041 libqom = static_library('qom', qom_ss.sources() + genh,
3042 dependencies: [qom_ss.dependencies()],
3044 qom = declare_dependency(link_whole: libqom)
3046 event_loop_base = files('event-loop-base.c')
3047 event_loop_base = static_library('event-loop-base', sources: event_loop_base + genh,
3048 build_by_default: true)
3049 event_loop_base = declare_dependency(link_whole: event_loop_base,
3050 dependencies: [qom])
3052 stub_ss = stub_ss.apply(config_all, strict: false)
3054 util_ss.add_all(trace_ss)
3055 util_ss = util_ss.apply(config_all, strict: false)
3056 libqemuutil = static_library('qemuutil',
3057 sources: util_ss.sources() + stub_ss.sources() + genh,
3058 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman])
3059 qemuutil = declare_dependency(link_with: libqemuutil,
3060 sources: genh + version_res,
3061 dependencies: [event_loop_base])
3063 if have_system or have_user
3064 decodetree = generator(find_program('scripts/decodetree.py'),
3065 output: 'decode-@BASENAME@.c.inc',
3066 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@'])
3067 subdir('libdecnumber')
3084 if config_host_data.get('CONFIG_REPLICATION')
3085 block_ss.add(files('replication.c'))
3092 blockdev_ss.add(files(
3099 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon,
3100 # os-win32.c does not
3101 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c'))
3102 softmmu_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')])
3105 common_ss.add(files('cpus-common.c'))
3109 common_ss.add(capstone)
3110 specific_ss.add(files('cpu.c', 'disas.c'), capstone)
3112 # Work around a gcc bug/misfeature wherein constant propagation looks
3114 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696
3115 # to guess that a const variable is always zero. Without lto, this is
3116 # impossible, as the alias is restricted to page-vary-common.c. Indeed,
3117 # without lto, not even the alias is required -- we simply use different
3118 # declarations in different compilation units.
3119 pagevary = files('page-vary-common.c')
3120 if get_option('b_lto')
3121 pagevary_flags = ['-fno-lto']
3122 if get_option('cfi')
3123 pagevary_flags += '-fno-sanitize=cfi-icall'
3125 pagevary = static_library('page-vary-common', sources: pagevary + genh,
3126 c_args: pagevary_flags)
3127 pagevary = declare_dependency(link_with: pagevary)
3129 common_ss.add(pagevary)
3130 specific_ss.add(files('page-vary.c'))
3138 subdir('semihosting')
3145 common_user_inc = []
3147 subdir('common-user')
3149 subdir('linux-user')
3151 # needed for fuzzing binaries
3152 subdir('tests/qtest/libqos')
3153 subdir('tests/qtest/fuzz')
3156 tcg_real_module_ss = ss.source_set()
3157 tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss)
3158 specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss)
3159 target_modules += { 'accel' : { 'qtest': qtest_module_ss,
3160 'tcg': tcg_real_module_ss }}
3162 ########################
3163 # Library dependencies #
3164 ########################
3166 modinfo_collect = find_program('scripts/modinfo-collect.py')
3167 modinfo_generate = find_program('scripts/modinfo-generate.py')
3172 foreach d, list : modules
3173 foreach m, module_ss : list
3174 if enable_modules and targetos != 'windows'
3175 module_ss = module_ss.apply(config_all, strict: false)
3176 sl = static_library(d + '-' + m, [genh, module_ss.sources()],
3177 dependencies: [modulecommon, module_ss.dependencies()], pic: true)
3183 if module_ss.sources() != []
3184 # FIXME: Should use sl.extract_all_objects(recursive: true) as
3185 # input. Sources can be used multiple times but objects are
3186 # unique when it comes to lookup in compile_commands.json.
3187 # Depnds on a mesion version with
3188 # https://github.com/mesonbuild/meson/pull/8900
3189 modinfo_files += custom_target(d + '-' + m + '.modinfo',
3190 output: d + '-' + m + '.modinfo',
3191 input: module_ss.sources() + genh,
3193 command: [modinfo_collect, module_ss.sources()])
3197 block_ss.add_all(module_ss)
3199 softmmu_ss.add_all(module_ss)
3205 foreach d, list : target_modules
3206 foreach m, module_ss : list
3207 if enable_modules and targetos != 'windows'
3208 foreach target : target_dirs
3209 if target.endswith('-softmmu')
3210 config_target = config_target_mak[target]
3211 config_target += config_host
3212 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3213 c_args = ['-DNEED_CPU_H',
3214 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3215 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3216 target_module_ss = module_ss.apply(config_target, strict: false)
3217 if target_module_ss.sources() != []
3218 module_name = d + '-' + m + '-' + config_target['TARGET_NAME']
3219 sl = static_library(module_name,
3220 [genh, target_module_ss.sources()],
3221 dependencies: [modulecommon, target_module_ss.dependencies()],
3222 include_directories: target_inc,
3226 # FIXME: Should use sl.extract_all_objects(recursive: true) too.
3227 modinfo_files += custom_target(module_name + '.modinfo',
3228 output: module_name + '.modinfo',
3229 input: target_module_ss.sources() + genh,
3231 command: [modinfo_collect, '--target', target, target_module_ss.sources()])
3236 specific_ss.add_all(module_ss)
3242 foreach target : target_dirs
3243 if target.endswith('-softmmu')
3244 config_target = config_target_mak[target]
3245 config_devices_mak = target + '-config-devices.mak'
3246 modinfo_src = custom_target('modinfo-' + target + '.c',
3247 output: 'modinfo-' + target + '.c',
3248 input: modinfo_files,
3249 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'],
3252 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src)
3253 modinfo_dep = declare_dependency(link_with: modinfo_lib)
3255 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH']
3256 hw_arch[arch].add(modinfo_dep)
3261 nm = find_program('nm')
3262 undefsym = find_program('scripts/undefsym.py')
3263 block_syms = custom_target('block.syms', output: 'block.syms',
3264 input: [libqemuutil, block_mods],
3266 command: [undefsym, nm, '@INPUT@'])
3267 qemu_syms = custom_target('qemu.syms', output: 'qemu.syms',
3268 input: [libqemuutil, softmmu_mods],
3270 command: [undefsym, nm, '@INPUT@'])
3272 authz_ss = authz_ss.apply(config_host, strict: false)
3273 libauthz = static_library('authz', authz_ss.sources() + genh,
3274 dependencies: [authz_ss.dependencies()],
3276 build_by_default: false)
3278 authz = declare_dependency(link_whole: libauthz,
3281 crypto_ss = crypto_ss.apply(config_host, strict: false)
3282 libcrypto = static_library('crypto', crypto_ss.sources() + genh,
3283 dependencies: [crypto_ss.dependencies()],
3285 build_by_default: false)
3287 crypto = declare_dependency(link_whole: libcrypto,
3288 dependencies: [authz, qom])
3290 io_ss = io_ss.apply(config_host, strict: false)
3291 libio = static_library('io', io_ss.sources() + genh,
3292 dependencies: [io_ss.dependencies()],
3293 link_with: libqemuutil,
3295 build_by_default: false)
3297 io = declare_dependency(link_whole: libio, dependencies: [crypto, qom])
3299 libmigration = static_library('migration', sources: migration_files + genh,
3301 build_by_default: false)
3302 migration = declare_dependency(link_with: libmigration,
3303 dependencies: [zlib, qom, io])
3304 softmmu_ss.add(migration)
3306 block_ss = block_ss.apply(config_host, strict: false)
3307 libblock = static_library('block', block_ss.sources() + genh,
3308 dependencies: block_ss.dependencies(),
3309 link_depends: block_syms,
3311 build_by_default: false)
3313 block = declare_dependency(link_whole: [libblock],
3314 link_args: '@block.syms',
3315 dependencies: [crypto, io])
3317 blockdev_ss = blockdev_ss.apply(config_host, strict: false)
3318 libblockdev = static_library('blockdev', blockdev_ss.sources() + genh,
3319 dependencies: blockdev_ss.dependencies(),
3321 build_by_default: false)
3323 blockdev = declare_dependency(link_whole: [libblockdev],
3324 dependencies: [block, event_loop_base])
3326 qmp_ss = qmp_ss.apply(config_host, strict: false)
3327 libqmp = static_library('qmp', qmp_ss.sources() + genh,
3328 dependencies: qmp_ss.dependencies(),
3330 build_by_default: false)
3332 qmp = declare_dependency(link_whole: [libqmp])
3334 libchardev = static_library('chardev', chardev_ss.sources() + genh,
3336 dependencies: chardev_ss.dependencies(),
3337 build_by_default: false)
3339 chardev = declare_dependency(link_whole: libchardev)
3341 hwcore_ss = hwcore_ss.apply(config_host, strict: false)
3342 libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh,
3344 build_by_default: false)
3345 hwcore = declare_dependency(link_whole: libhwcore)
3346 common_ss.add(hwcore)
3352 emulator_modules = []
3353 foreach m : block_mods + softmmu_mods
3354 emulator_modules += shared_module(m.name(),
3355 build_by_default: true,
3359 install_dir: qemu_moddir)
3361 if emulator_modules.length() > 0
3362 alias_target('modules', emulator_modules)
3365 softmmu_ss.add(authz, blockdev, chardev, crypto, io, qmp)
3366 common_ss.add(qom, qemuutil)
3368 common_ss.add_all(when: 'CONFIG_SOFTMMU', if_true: [softmmu_ss])
3369 common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss)
3371 common_all = common_ss.apply(config_all, strict: false)
3372 common_all = static_library('common',
3373 build_by_default: false,
3374 sources: common_all.sources() + genh,
3375 include_directories: common_user_inc,
3376 implicit_include_directories: false,
3377 dependencies: common_all.dependencies(),
3380 feature_to_c = find_program('scripts/feature_to_c.sh')
3382 if targetos == 'darwin'
3383 entitlement = find_program('scripts/entitlement.sh')
3387 foreach target : target_dirs
3388 config_target = config_target_mak[target]
3389 target_name = config_target['TARGET_NAME']
3390 target_base_arch = config_target['TARGET_BASE_ARCH']
3391 arch_srcs = [config_target_h[target]]
3393 c_args = ['-DNEED_CPU_H',
3394 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3395 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3396 link_args = emulator_link_args
3398 config_target += config_host
3399 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3400 if targetos == 'linux'
3401 target_inc += include_directories('linux-headers', is_system: true)
3403 if target.endswith('-softmmu')
3404 target_type='system'
3405 t = target_softmmu_arch[target_base_arch].apply(config_target, strict: false)
3406 arch_srcs += t.sources()
3407 arch_deps += t.dependencies()
3409 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch
3410 hw = hw_arch[hw_dir].apply(config_target, strict: false)
3411 arch_srcs += hw.sources()
3412 arch_deps += hw.dependencies()
3414 arch_srcs += config_devices_h[target]
3415 link_args += ['@block.syms', '@qemu.syms']
3417 abi = config_target['TARGET_ABI_DIR']
3419 target_inc += common_user_inc
3420 if target_base_arch in target_user_arch
3421 t = target_user_arch[target_base_arch].apply(config_target, strict: false)
3422 arch_srcs += t.sources()
3423 arch_deps += t.dependencies()
3425 if 'CONFIG_LINUX_USER' in config_target
3426 base_dir = 'linux-user'
3428 if 'CONFIG_BSD_USER' in config_target
3429 base_dir = 'bsd-user'
3430 target_inc += include_directories('bsd-user/' / targetos)
3431 target_inc += include_directories('bsd-user/host/' / host_arch)
3432 dir = base_dir / abi
3433 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c')
3435 target_inc += include_directories(
3439 if 'CONFIG_LINUX_USER' in config_target
3440 dir = base_dir / abi
3441 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c')
3442 if config_target.has_key('TARGET_SYSTBL_ABI')
3444 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'],
3445 extra_args : config_target['TARGET_SYSTBL_ABI'])
3450 if 'TARGET_XML_FILES' in config_target
3451 gdbstub_xml = custom_target(target + '-gdbstub-xml.c',
3452 output: target + '-gdbstub-xml.c',
3453 input: files(config_target['TARGET_XML_FILES'].split()),
3454 command: [feature_to_c, '@INPUT@'],
3456 arch_srcs += gdbstub_xml
3459 t = target_arch[target_base_arch].apply(config_target, strict: false)
3460 arch_srcs += t.sources()
3461 arch_deps += t.dependencies()
3463 target_common = common_ss.apply(config_target, strict: false)
3464 objects = common_all.extract_objects(target_common.sources())
3465 deps = target_common.dependencies()
3467 target_specific = specific_ss.apply(config_target, strict: false)
3468 arch_srcs += target_specific.sources()
3469 arch_deps += target_specific.dependencies()
3471 lib = static_library('qemu-' + target,
3472 sources: arch_srcs + genh,
3473 dependencies: arch_deps,
3475 include_directories: target_inc,
3477 build_by_default: false,
3480 if target.endswith('-softmmu')
3482 'name': 'qemu-system-' + target_name,
3483 'win_subsystem': 'console',
3484 'sources': files('softmmu/main.c'),
3487 if targetos == 'windows' and (sdl.found() or gtk.found())
3489 'name': 'qemu-system-' + target_name + 'w',
3490 'win_subsystem': 'windows',
3491 'sources': files('softmmu/main.c'),
3495 if get_option('fuzzing')
3496 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false)
3498 'name': 'qemu-fuzz-' + target_name,
3499 'win_subsystem': 'console',
3500 'sources': specific_fuzz.sources(),
3501 'dependencies': specific_fuzz.dependencies(),
3506 'name': 'qemu-' + target_name,
3507 'win_subsystem': 'console',
3513 exe_name = exe['name']
3514 if targetos == 'darwin'
3515 exe_name += '-unsigned'
3518 emulator = executable(exe_name, exe['sources'],
3521 dependencies: arch_deps + deps + exe['dependencies'],
3522 objects: lib.extract_all_objects(recursive: true),
3523 link_language: link_language,
3524 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []),
3525 link_args: link_args,
3526 win_subsystem: exe['win_subsystem'])
3528 if targetos == 'darwin'
3529 icon = 'pc-bios/qemu.rsrc'
3530 build_input = [emulator, files(icon)]
3532 get_option('bindir') / exe_name,
3533 meson.current_source_dir() / icon
3535 if 'CONFIG_HVF' in config_target
3536 entitlements = 'accel/hvf/entitlements.plist'
3537 build_input += files(entitlements)
3538 install_input += meson.current_source_dir() / entitlements
3541 emulators += {exe['name'] : custom_target(exe['name'],
3543 output: exe['name'],
3544 command: [entitlement, '@OUTPUT@', '@INPUT@'])
3547 meson.add_install_script(entitlement, '--install',
3548 get_option('bindir') / exe['name'],
3551 emulators += {exe['name']: emulator}
3556 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false},
3557 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true},
3558 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true},
3559 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true},
3561 custom_target(exe['name'] + stp['ext'],
3562 input: trace_events_all,
3563 output: exe['name'] + stp['ext'],
3564 install: stp['install'],
3565 install_dir: get_option('datadir') / 'systemtap/tapset',
3567 tracetool, '--group=all', '--format=' + stp['fmt'],
3568 '--binary=' + stp['bin'],
3569 '--target-name=' + target_name,
3570 '--target-type=' + target_type,
3571 '--probe-prefix=qemu.' + target_type + '.' + target_name,
3572 '@INPUT@', '@OUTPUT@'
3574 depend_files: tracetool_depends)
3580 # Other build targets
3582 if 'CONFIG_PLUGIN' in config_host
3583 install_headers('include/qemu/qemu-plugin.h')
3588 # Don't build qemu-keymap if xkbcommon is not explicitly enabled
3589 # when we don't build tools or system
3590 if xkbcommon.found()
3591 # used for the update-keymaps target, so include rules even if !have_tools
3592 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh,
3593 dependencies: [qemuutil, xkbcommon], install: have_tools)
3597 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep],
3598 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true)
3599 qemu_io = executable('qemu-io', files('qemu-io.c'),
3600 dependencies: [block, qemuutil], install: true)
3601 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'),
3602 dependencies: [blockdev, qemuutil, gnutls, selinux],
3605 subdir('storage-daemon')
3606 subdir('contrib/rdmacm-mux')
3607 subdir('contrib/elf2dmp')
3609 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'),
3610 dependencies: qemuutil,
3614 subdir('contrib/vhost-user-blk')
3615 subdir('contrib/vhost-user-gpu')
3616 subdir('contrib/vhost-user-input')
3617 subdir('contrib/vhost-user-scsi')
3620 if targetos == 'linux'
3621 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'),
3622 dependencies: [qemuutil, libcap_ng],
3624 install_dir: get_option('libexecdir'))
3626 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'),
3627 dependencies: [authz, crypto, io, qom, qemuutil,
3628 libcap_ng, mpathpersist],
3633 subdir('contrib/ivshmem-client')
3634 subdir('contrib/ivshmem-server')
3647 if host_machine.system() == 'windows'
3649 find_program('scripts/nsis.py'),
3651 get_option('prefix'),
3652 meson.current_source_dir(),
3653 config_host['GLIB_BINDIR'],
3656 '-DDISPLAYVERSION=' + meson.project_version(),
3659 nsis_cmd += '-DCONFIG_DOCUMENTATION=y'
3662 nsis_cmd += '-DCONFIG_GTK=y'
3665 nsis = custom_target('nsis',
3666 output: 'qemu-setup-' + meson.project_version() + '.exe',
3667 input: files('qemu.nsi'),
3668 build_always_stale: true,
3669 command: nsis_cmd + ['@INPUT@'])
3670 alias_target('installer', nsis)
3673 #########################
3674 # Configuration summary #
3675 #########################
3679 summary_info += {'Install prefix': get_option('prefix')}
3680 summary_info += {'BIOS directory': qemu_datadir}
3681 pathsep = targetos == 'windows' ? ';' : ':'
3682 summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))}
3683 summary_info += {'binary directory': get_option('prefix') / get_option('bindir')}
3684 summary_info += {'library directory': get_option('prefix') / get_option('libdir')}
3685 summary_info += {'module directory': qemu_moddir}
3686 summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')}
3687 summary_info += {'include directory': get_option('prefix') / get_option('includedir')}
3688 summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')}
3689 if targetos != 'windows'
3690 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')}
3691 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')}
3693 summary_info += {'local state directory': 'queried at runtime'}
3695 summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')}
3696 summary_info += {'Build directory': meson.current_build_dir()}
3697 summary_info += {'Source path': meson.current_source_dir()}
3698 summary_info += {'GIT submodules': config_host['GIT_SUBMODULES']}
3699 summary(summary_info, bool_yn: true, section: 'Directories')
3703 summary_info += {'git': config_host['GIT']}
3704 summary_info += {'make': config_host['MAKE']}
3705 summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())}
3706 summary_info += {'sphinx-build': sphinx_build}
3707 if config_host.has_key('HAVE_GDB_BIN')
3708 summary_info += {'gdb': config_host['HAVE_GDB_BIN']}
3710 summary_info += {'iasl': iasl}
3711 summary_info += {'genisoimage': config_host['GENISOIMAGE']}
3712 if targetos == 'windows' and have_ga
3713 summary_info += {'wixl': wixl}
3715 if slirp.found() and have_system
3716 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false}
3718 summary(summary_info, bool_yn: true, section: 'Host binaries')
3720 # Configurable features
3722 summary_info += {'Documentation': build_docs}
3723 summary_info += {'system-mode emulation': have_system}
3724 summary_info += {'user-mode emulation': have_user}
3725 summary_info += {'block layer': have_block}
3726 summary_info += {'Install blobs': get_option('install_blobs')}
3727 summary_info += {'module support': config_host.has_key('CONFIG_MODULES')}
3728 if config_host.has_key('CONFIG_MODULES')
3729 summary_info += {'alternative module path': get_option('module_upgrades')}
3731 summary_info += {'fuzzing support': get_option('fuzzing')}
3733 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)}
3735 summary_info += {'Trace backends': ','.join(get_option('trace_backends'))}
3736 if 'simple' in get_option('trace_backends')
3737 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'}
3739 summary_info += {'D-Bus display': dbus_display}
3740 summary_info += {'QOM debugging': get_option('qom_cast_debug')}
3741 summary_info += {'vhost-kernel support': have_vhost_kernel}
3742 summary_info += {'vhost-net support': have_vhost_net}
3743 summary_info += {'vhost-user support': have_vhost_user}
3744 summary_info += {'vhost-user-crypto support': have_vhost_user_crypto}
3745 summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server}
3746 summary_info += {'vhost-vdpa support': have_vhost_vdpa}
3747 summary_info += {'build guest agent': have_ga}
3748 summary(summary_info, bool_yn: true, section: 'Configurable features')
3750 # Compilation information
3752 summary_info += {'host CPU': cpu}
3753 summary_info += {'host endianness': build_machine.endian()}
3754 summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())}
3755 summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())}
3756 if link_language == 'cpp'
3757 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())}
3759 summary_info += {'C++ compiler': false}
3761 if targetos == 'darwin'
3762 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())}
3764 option_cflags = (get_option('debug') ? ['-g'] : [])
3765 if get_option('optimization') != 'plain'
3766 option_cflags += ['-O' + get_option('optimization')]
3768 summary_info += {'CFLAGS': ' '.join(get_option('c_args') + option_cflags)}
3769 if link_language == 'cpp'
3770 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args') + option_cflags)}
3772 if targetos == 'darwin'
3773 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args') + option_cflags)}
3775 link_args = get_option(link_language + '_link_args')
3776 if link_args.length() > 0
3777 summary_info += {'LDFLAGS': ' '.join(link_args)}
3779 summary_info += {'QEMU_CFLAGS': ' '.join(qemu_cflags)}
3780 if 'cpp' in all_languages
3781 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_cxxflags)}
3783 if 'objc' in all_languages
3784 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_objcflags)}
3786 summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)}
3787 summary_info += {'profiler': get_option('profiler')}
3788 summary_info += {'link-time optimization (LTO)': get_option('b_lto')}
3789 summary_info += {'PIE': get_option('b_pie')}
3790 summary_info += {'static build': config_host.has_key('CONFIG_STATIC')}
3791 summary_info += {'malloc trim support': has_malloc_trim}
3792 summary_info += {'membarrier': have_membarrier}
3793 summary_info += {'debug stack usage': get_option('debug_stack_usage')}
3794 summary_info += {'mutex debugging': get_option('debug_mutex')}
3795 summary_info += {'memory allocator': get_option('malloc')}
3796 summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')}
3797 summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')}
3798 summary_info += {'gprof enabled': get_option('gprof')}
3799 summary_info += {'gcov': get_option('b_coverage')}
3800 summary_info += {'thread sanitizer': config_host.has_key('CONFIG_TSAN')}
3801 summary_info += {'CFI support': get_option('cfi')}
3802 if get_option('cfi')
3803 summary_info += {'CFI debug support': get_option('cfi_debug')}
3805 summary_info += {'strip binaries': get_option('strip')}
3806 summary_info += {'sparse': sparse}
3807 summary_info += {'mingw32 support': targetos == 'windows'}
3808 summary(summary_info, bool_yn: true, section: 'Compilation')
3810 # snarf the cross-compilation information for tests
3813 foreach target: target_dirs
3814 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak'
3815 if fs.exists(tcg_mak)
3816 config_cross_tcg = keyval.load(tcg_mak)
3817 if 'CC' in config_cross_tcg
3818 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']}
3824 summary(summary_info, bool_yn: true, section: 'Cross compilers')
3827 # Targets and accelerators
3830 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')}
3831 summary_info += {'HAX support': config_all.has_key('CONFIG_HAX')}
3832 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')}
3833 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')}
3834 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')}
3835 summary_info += {'Xen support': xen.found()}
3837 summary_info += {'xen ctrl version': xen.version()}
3840 summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')}
3841 if config_all.has_key('CONFIG_TCG')
3842 if get_option('tcg_interpreter')
3843 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'}
3845 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)}
3847 summary_info += {'TCG plugins': config_host.has_key('CONFIG_PLUGIN')}
3848 summary_info += {'TCG debug enabled': config_host.has_key('CONFIG_DEBUG_TCG')}
3850 summary_info += {'target list': ' '.join(target_dirs)}
3852 summary_info += {'default devices': get_option('default_devices')}
3853 summary_info += {'out of process emulation': multiprocess_allowed}
3854 summary_info += {'vfio-user server': vfio_user_server_allowed}
3856 summary(summary_info, bool_yn: true, section: 'Targets and accelerators')
3860 summary_info += {'coroutine backend': config_host['CONFIG_COROUTINE_BACKEND']}
3861 summary_info += {'coroutine pool': have_coroutine_pool}
3863 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')}
3864 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')}
3865 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')}
3866 summary_info += {'VirtFS support': have_virtfs}
3867 summary_info += {'build virtiofs daemon': have_virtiofsd}
3868 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')}
3869 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')}
3870 summary_info += {'bochs support': get_option('bochs').allowed()}
3871 summary_info += {'cloop support': get_option('cloop').allowed()}
3872 summary_info += {'dmg support': get_option('dmg').allowed()}
3873 summary_info += {'qcow v1 support': get_option('qcow1').allowed()}
3874 summary_info += {'vdi support': get_option('vdi').allowed()}
3875 summary_info += {'vvfat support': get_option('vvfat').allowed()}
3876 summary_info += {'qed support': get_option('qed').allowed()}
3877 summary_info += {'parallels support': get_option('parallels').allowed()}
3878 summary_info += {'FUSE exports': fuse}
3879 summary_info += {'VDUSE block exports': have_vduse_blk_export}
3881 summary(summary_info, bool_yn: true, section: 'Block layer support')
3885 summary_info += {'TLS priority': get_option('tls_priority')}
3886 summary_info += {'GNUTLS support': gnutls}
3888 summary_info += {' GNUTLS crypto': gnutls_crypto.found()}
3890 summary_info += {'libgcrypt': gcrypt}
3891 summary_info += {'nettle': nettle}
3893 summary_info += {' XTS': xts != 'private'}
3895 summary_info += {'AF_ALG support': have_afalg}
3896 summary_info += {'rng-none': get_option('rng_none')}
3897 summary_info += {'Linux keyring': have_keyring}
3898 summary(summary_info, bool_yn: true, section: 'Crypto')
3902 if targetos == 'darwin'
3903 summary_info += {'Cocoa support': cocoa}
3904 summary_info += {'vmnet.framework support': vmnet}
3906 summary_info += {'SDL support': sdl}
3907 summary_info += {'SDL image support': sdl_image}
3908 summary_info += {'GTK support': gtk}
3909 summary_info += {'pixman': pixman}
3910 summary_info += {'VTE support': vte}
3911 summary_info += {'slirp support': slirp}
3912 summary_info += {'libtasn1': tasn1}
3913 summary_info += {'PAM': pam}
3914 summary_info += {'iconv support': iconv}
3915 summary_info += {'curses support': curses}
3916 summary_info += {'virgl support': virgl}
3917 summary_info += {'blkio support': blkio}
3918 summary_info += {'curl support': curl}
3919 summary_info += {'Multipath support': mpathpersist}
3920 summary_info += {'PNG support': png}
3921 summary_info += {'VNC support': vnc}
3923 summary_info += {'VNC SASL support': sasl}
3924 summary_info += {'VNC JPEG support': jpeg}
3926 if targetos not in ['darwin', 'haiku', 'windows']
3927 summary_info += {'OSS support': oss}
3928 summary_info += {'sndio support': sndio}
3929 elif targetos == 'darwin'
3930 summary_info += {'CoreAudio support': coreaudio}
3931 elif targetos == 'windows'
3932 summary_info += {'DirectSound support': dsound}
3934 if targetos == 'linux'
3935 summary_info += {'ALSA support': alsa}
3936 summary_info += {'PulseAudio support': pulse}
3938 summary_info += {'JACK support': jack}
3939 summary_info += {'brlapi support': brlapi}
3940 summary_info += {'vde support': vde}
3941 summary_info += {'netmap support': have_netmap}
3942 summary_info += {'l2tpv3 support': have_l2tpv3}
3943 summary_info += {'Linux AIO support': libaio}
3944 summary_info += {'Linux io_uring support': linux_io_uring}
3945 summary_info += {'ATTR/XATTR support': libattr}
3946 summary_info += {'RDMA support': rdma}
3947 summary_info += {'PVRDMA support': have_pvrdma}
3948 summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt}
3949 summary_info += {'libcap-ng support': libcap_ng}
3950 summary_info += {'bpf support': libbpf}
3951 summary_info += {'spice protocol support': spice_protocol}
3952 if spice_protocol.found()
3953 summary_info += {' spice server support': spice}
3955 summary_info += {'rbd support': rbd}
3956 summary_info += {'smartcard support': cacard}
3957 summary_info += {'U2F support': u2f}
3958 summary_info += {'libusb': libusb}
3959 summary_info += {'usb net redir': usbredir}
3960 summary_info += {'OpenGL support (epoxy)': opengl}
3961 summary_info += {'GBM': gbm}
3962 summary_info += {'libiscsi support': libiscsi}
3963 summary_info += {'libnfs support': libnfs}
3964 if targetos == 'windows'
3966 summary_info += {'QGA VSS support': have_qga_vss}
3969 summary_info += {'seccomp support': seccomp}
3970 summary_info += {'GlusterFS support': glusterfs}
3971 summary_info += {'TPM support': have_tpm}
3972 summary_info += {'libssh support': libssh}
3973 summary_info += {'lzo support': lzo}
3974 summary_info += {'snappy support': snappy}
3975 summary_info += {'bzip2 support': libbzip2}
3976 summary_info += {'lzfse support': liblzfse}
3977 summary_info += {'zstd support': zstd}
3978 summary_info += {'NUMA host support': numa}
3979 summary_info += {'capstone': capstone}
3980 summary_info += {'libpmem support': libpmem}
3981 summary_info += {'libdaxctl support': libdaxctl}
3982 summary_info += {'libudev': libudev}
3983 # Dummy dependency, keep .found()
3984 summary_info += {'FUSE lseek': fuse_lseek.found()}
3985 summary_info += {'selinux': selinux}
3986 summary(summary_info, bool_yn: true, section: 'Dependencies')
3988 if not supported_cpus.contains(cpu)
3990 warning('SUPPORT FOR THIS HOST CPU WILL GO AWAY IN FUTURE RELEASES!')
3992 message('CPU host architecture ' + cpu + ' support is not currently maintained.')
3993 message('The QEMU project intends to remove support for this host CPU in')
3994 message('a future release if nobody volunteers to maintain it and to')
3995 message('provide a build host for our continuous integration setup.')
3996 message('configure has succeeded and you can continue to build, but')
3997 message('if you care about QEMU on this platform you should contact')
3998 message('us upstream at qemu-devel@nongnu.org.')
4001 if not supported_oses.contains(targetos)
4003 warning('WARNING: SUPPORT FOR THIS HOST OS WILL GO AWAY IN FUTURE RELEASES!')
4005 message('Host OS ' + targetos + 'support is not currently maintained.')
4006 message('The QEMU project intends to remove support for this host OS in')
4007 message('a future release if nobody volunteers to maintain it and to')
4008 message('provide a build host for our continuous integration setup.')
4009 message('configure has succeeded and you can continue to build, but')
4010 message('if you care about QEMU on this platform you should contact')
4011 message('us upstream at qemu-devel@nongnu.org.')