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 sh = find_program('sh')
18 cc = meson.get_compiler('c')
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 # Temporary directory used for files created while
27 # configure runs. Since it is in the build directory
28 # we can safely blow away any previous version of it
29 # (and we need not jump through hoops to try to delete
30 # it when configure exits.)
31 tmpdir = meson.current_build_dir() / 'meson-private/temp'
33 if get_option('qemu_suffix').startswith('/')
34 error('qemu_suffix cannot start with a /')
37 qemu_confdir = get_option('sysconfdir') / get_option('qemu_suffix')
38 qemu_datadir = get_option('datadir') / get_option('qemu_suffix')
39 qemu_docdir = get_option('docdir') / get_option('qemu_suffix')
40 qemu_moddir = get_option('libdir') / get_option('qemu_suffix')
42 qemu_desktopdir = get_option('datadir') / 'applications'
43 qemu_icondir = get_option('datadir') / 'icons'
45 config_host_data = configuration_data()
47 qapi_trace_events = []
49 bsd_oses = ['gnu/kfreebsd', 'freebsd', 'netbsd', 'openbsd', 'dragonfly', 'darwin']
50 supported_oses = ['windows', 'freebsd', 'netbsd', 'openbsd', 'darwin', 'sunos', 'linux']
51 supported_cpus = ['ppc', 'ppc64', 's390x', 'riscv', 'x86', 'x86_64',
52 'arm', 'aarch64', 'loongarch64', 'mips', 'mips64', 'sparc64']
54 cpu = host_machine.cpu_family()
56 # Unify riscv* to a single family.
57 if cpu in ['riscv32', 'riscv64']
61 targetos = host_machine.system()
63 target_dirs = config_host['TARGET_DIRS'].split()
64 have_linux_user = false
67 foreach target : target_dirs
68 have_linux_user = have_linux_user or target.endswith('linux-user')
69 have_bsd_user = have_bsd_user or target.endswith('bsd-user')
70 have_system = have_system or target.endswith('-softmmu')
72 have_user = have_linux_user or have_bsd_user
73 have_tools = get_option('tools') \
74 .disable_auto_if(not have_system) \
76 have_ga = get_option('guest_agent') \
77 .disable_auto_if(not have_system and not have_tools) \
78 .require(targetos in ['sunos', 'linux', 'windows', 'freebsd'],
79 error_message: 'unsupported OS for QEMU guest agent') \
81 have_block = have_system or have_tools
83 python = import('python').find_installation()
85 if cpu not in supported_cpus
95 if cpu in ['x86', 'x86_64']
96 kvm_targets = ['i386-softmmu', 'x86_64-softmmu']
98 kvm_targets = ['aarch64-softmmu']
100 kvm_targets = ['s390x-softmmu']
101 elif cpu in ['ppc', 'ppc64']
102 kvm_targets = ['ppc-softmmu', 'ppc64-softmmu']
103 elif cpu in ['mips', 'mips64']
104 kvm_targets = ['mips-softmmu', 'mipsel-softmmu', 'mips64-softmmu', 'mips64el-softmmu']
105 elif cpu in ['riscv']
106 kvm_targets = ['riscv32-softmmu', 'riscv64-softmmu']
112 if get_option('kvm').allowed() and targetos == 'linux'
113 kvm_targets_c = '"' + '" ,"'.join(kvm_targets) + '"'
115 config_host_data.set('CONFIG_KVM_TARGETS', kvm_targets_c)
117 accelerator_targets = { 'CONFIG_KVM': kvm_targets }
119 if cpu in ['aarch64']
120 accelerator_targets += {
121 'CONFIG_HVF': ['aarch64-softmmu']
125 if cpu in ['x86', 'x86_64', 'arm', 'aarch64']
126 # i386 emulator provides xenpv machine type for multiple architectures
127 accelerator_targets += {
128 'CONFIG_XEN': ['i386-softmmu', 'x86_64-softmmu'],
131 if cpu in ['x86', 'x86_64']
132 accelerator_targets += {
133 'CONFIG_HAX': ['i386-softmmu', 'x86_64-softmmu'],
134 'CONFIG_HVF': ['x86_64-softmmu'],
135 'CONFIG_NVMM': ['i386-softmmu', 'x86_64-softmmu'],
136 'CONFIG_WHPX': ['i386-softmmu', 'x86_64-softmmu'],
141 # Darwin does not support references to thread-local variables in modules
142 if targetos != 'darwin'
143 modular_tcg = ['i386-softmmu', 'x86_64-softmmu']
146 edk2_targets = [ 'arm-softmmu', 'aarch64-softmmu', 'i386-softmmu', 'x86_64-softmmu' ]
147 unpack_edk2_blobs = false
148 foreach target : edk2_targets
149 if target in target_dirs
150 bzip2 = find_program('bzip2', required: get_option('install_blobs'))
151 unpack_edk2_blobs = bzip2.found()
158 if 'dtrace' in get_option('trace_backends')
159 dtrace = find_program('dtrace', required: true)
160 stap = find_program('stap', required: false)
162 # Workaround to avoid dtrace(1) producing a file with 'hidden' symbol
163 # visibility. Define STAP_SDT_V2 to produce 'default' symbol visibility
164 # instead. QEMU --enable-modules depends on this because the SystemTap
165 # semaphores are linked into the main binary and not the module's shared
167 add_global_arguments('-DSTAP_SDT_V2',
168 native: false, language: ['c', 'cpp', 'objc'])
172 if get_option('iasl') == ''
173 iasl = find_program('iasl', required: false)
175 iasl = find_program(get_option('iasl'), required: true)
182 qemu_cflags = config_host['QEMU_CFLAGS'].split()
183 qemu_objcflags = config_host['QEMU_OBJCFLAGS'].split()
184 qemu_ldflags = config_host['QEMU_LDFLAGS'].split()
187 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static'
190 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
191 # The combination is known as "full relro", because .got.plt is read-only too.
192 qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now')
194 if targetos == 'windows'
195 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--no-seh', '-Wl,--nxcompat')
196 # Disable ASLR for debug builds to allow debugging with gdb
197 if get_option('optimization') == '0'
198 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--dynamicbase')
202 if get_option('gprof')
203 qemu_cflags += ['-p']
204 qemu_objcflags += ['-p']
205 qemu_ldflags += ['-p']
208 # Specify linker-script with add_project_link_arguments so that it is not placed
209 # within a linker --start-group/--end-group pair
210 if get_option('fuzzing')
211 add_project_link_arguments(['-Wl,-T,',
212 (meson.current_source_dir() / 'tests/qtest/fuzz/fork_fuzz.ld')],
213 native: false, language: ['c', 'cpp', 'objc'])
215 # Specify a filter to only instrument code that is directly related to
217 configure_file(output: 'instrumentation-filter',
218 input: 'scripts/oss-fuzz/instrumentation-filter-template',
221 if cc.compiles('int main () { return 0; }',
222 name: '-fsanitize-coverage-allowlist=/dev/null',
223 args: ['-fsanitize-coverage-allowlist=/dev/null',
224 '-fsanitize-coverage=trace-pc'] )
225 add_global_arguments('-fsanitize-coverage-allowlist=instrumentation-filter',
226 native: false, language: ['c', 'cpp', 'objc'])
229 if get_option('fuzzing_engine') == ''
230 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the
231 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link
232 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be
233 # unable to bind the fuzzer-related callbacks added by instrumentation.
234 add_global_arguments('-fsanitize=fuzzer-no-link',
235 native: false, language: ['c', 'cpp', 'objc'])
236 add_global_link_arguments('-fsanitize=fuzzer-no-link',
237 native: false, language: ['c', 'cpp', 'objc'])
238 # For the actual fuzzer binaries, we need to link against the libfuzzer
239 # library. They need to be configurable, to support OSS-Fuzz
240 fuzz_exe_ldflags = ['-fsanitize=fuzzer']
242 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and
243 # the needed CFLAGS have already been provided
244 fuzz_exe_ldflags = get_option('fuzzing_engine').split()
248 add_global_arguments(qemu_cflags, native: false, language: ['c'])
249 add_global_arguments(qemu_objcflags, native: false, language: ['objc'])
251 # Check that the C++ compiler exists and works with the C compiler.
255 if add_languages('cpp', required: false, native: false)
256 cxx = meson.get_compiler('cpp')
257 add_global_arguments(['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'],
258 native: false, language: 'cpp')
259 foreach k: qemu_cflags
260 if k not in ['-Wstrict-prototypes', '-Wmissing-prototypes', '-Wnested-externs',
261 '-Wold-style-declaration', '-Wold-style-definition', '-Wredundant-decls']
265 add_global_arguments(qemu_cxxflags, native: false, language: 'cpp')
267 if cxx.links(files('scripts/main.c'), args: qemu_cflags)
268 link_language = 'cpp'
271 message('C++ compiler does not work with C compiler')
272 message('Disabling C++-specific optional code')
276 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
277 if targetos != 'sunos' and not config_host.has_key('CONFIG_TSAN')
278 qemu_ldflags += linker.get_supported_link_arguments('-Wl,--warn-common')
281 add_global_link_arguments(qemu_ldflags, native: false, language: ['c', 'cpp', 'objc'])
283 if targetos == 'linux'
284 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers',
285 '-isystem', 'linux-headers',
286 language: ['c', 'cpp'])
289 add_project_arguments('-iquote', '.',
290 '-iquote', meson.current_source_dir(),
291 '-iquote', meson.current_source_dir() / 'include',
292 language: ['c', 'cpp', 'objc'])
294 if host_machine.system() == 'darwin'
295 add_languages('objc', required: false, native: false)
298 sparse = find_program('cgcc', required: get_option('sparse'))
301 command: [find_program('scripts/check_sparse.py'),
302 'compile_commands.json', sparse.full_path(), '-Wbitwise',
303 '-Wno-transparent-union', '-Wno-old-initializer',
304 '-Wno-non-pointer-null'])
307 ###########################################
308 # Target-specific checks and dependencies #
309 ###########################################
312 if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \
315 #include <sys/types.h>
316 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
317 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
319 args: ['-Werror', '-fsanitize=fuzzer'])
320 error('Your compiler does not support -fsanitize=fuzzer')
324 if 'ftrace' in get_option('trace_backends') and targetos != 'linux'
325 error('ftrace is supported only on Linux')
327 if 'syslog' in get_option('trace_backends') and not cc.compiles('''
330 openlog("qemu", LOG_PID, LOG_DAEMON);
331 syslog(LOG_INFO, "configure");
334 error('syslog is not supported on this system')
337 # Miscellaneous Linux-only features
338 get_option('mpath') \
339 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux')
341 multiprocess_allowed = get_option('multiprocess') \
342 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \
345 vfio_user_server_allowed = get_option('vfio_user_server') \
346 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \
349 have_tpm = get_option('tpm') \
350 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \
354 have_vhost_user = get_option('vhost_user') \
355 .disable_auto_if(targetos != 'linux') \
356 .require(targetos != 'windows',
357 error_message: 'vhost-user is not available on Windows').allowed()
358 have_vhost_vdpa = get_option('vhost_vdpa') \
359 .require(targetos == 'linux',
360 error_message: 'vhost-vdpa is only available on Linux').allowed()
361 have_vhost_kernel = get_option('vhost_kernel') \
362 .require(targetos == 'linux',
363 error_message: 'vhost-kernel is only available on Linux').allowed()
364 have_vhost_user_crypto = get_option('vhost_crypto') \
365 .require(have_vhost_user,
366 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed()
368 have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel
370 have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed()
371 have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed()
372 have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed()
373 have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa
375 # Target-specific libraries and flags
376 libm = cc.find_library('m', required: false)
377 threads = dependency('threads')
378 util = cc.find_library('util', required: false)
384 emulator_link_args = []
391 if targetos == 'windows'
392 midl = find_program('midl', required: false)
393 widl = find_program('widl', required: false)
394 pathcch = cc.find_library('pathcch')
395 socket = cc.find_library('ws2_32')
396 winmm = cc.find_library('winmm')
398 win = import('windows')
399 version_res = win.compile_resources('version.rc',
400 depend_files: files('pc-bios/qemu-nsis.ico'),
401 include_directories: include_directories('.'))
403 elif targetos == 'darwin'
404 coref = dependency('appleframeworks', modules: 'CoreFoundation')
405 iokit = dependency('appleframeworks', modules: 'IOKit', required: false)
406 host_dsosuf = '.dylib'
407 elif targetos == 'sunos'
408 socket = [cc.find_library('socket'),
409 cc.find_library('nsl'),
410 cc.find_library('resolv')]
411 elif targetos == 'haiku'
412 socket = [cc.find_library('posix_error_mapper'),
413 cc.find_library('network'),
414 cc.find_library('bsd')]
415 elif targetos == 'openbsd'
416 if get_option('tcg').allowed() and target_dirs.length() > 0
417 # Disable OpenBSD W^X if available
418 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded')
422 # Target-specific configuration of accelerators
424 if get_option('kvm').allowed() and targetos == 'linux'
425 accelerators += 'CONFIG_KVM'
427 if get_option('whpx').allowed() and targetos == 'windows'
428 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64'
429 error('WHPX requires 64-bit host')
430 elif cc.has_header('WinHvPlatform.h', required: get_option('whpx')) and \
431 cc.has_header('WinHvEmulation.h', required: get_option('whpx'))
432 accelerators += 'CONFIG_WHPX'
435 if get_option('hvf').allowed()
436 hvf = dependency('appleframeworks', modules: 'Hypervisor',
437 required: get_option('hvf'))
439 accelerators += 'CONFIG_HVF'
442 if get_option('hax').allowed()
443 if get_option('hax').enabled() or targetos in ['windows', 'darwin', 'netbsd']
444 accelerators += 'CONFIG_HAX'
447 if targetos == 'netbsd'
448 nvmm = cc.find_library('nvmm', required: get_option('nvmm'))
450 accelerators += 'CONFIG_NVMM'
455 if get_option('tcg').allowed()
456 if host_arch == 'unknown'
457 if get_option('tcg_interpreter')
458 warning('Unsupported CPU @0@, will use TCG with TCI (slow)'.format(cpu))
460 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu))
462 elif get_option('tcg_interpreter')
463 warning('Use of the TCG interpreter is not recommended on this host')
464 warning('architecture. There is a native TCG execution backend available')
465 warning('which provides substantially better performance and reliability.')
466 warning('It is strongly recommended to remove the --enable-tcg-interpreter')
467 warning('configuration option on this architecture to use the native')
470 if get_option('tcg_interpreter')
472 elif host_arch == 'x86_64'
474 elif host_arch == 'ppc64'
477 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch,
478 language: ['c', 'cpp', 'objc'])
480 accelerators += 'CONFIG_TCG'
481 config_host += { 'CONFIG_TCG': 'y' }
484 if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled()
485 error('KVM not available on this platform')
487 if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled()
488 error('HVF not available on this platform')
490 if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled()
491 error('NVMM not available on this platform')
493 if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled()
494 error('WHPX not available on this platform')
501 # The path to glib.h is added to all compilation commands. This was
502 # grandfathered in from the QEMU Makefiles.
503 add_project_arguments(config_host['GLIB_CFLAGS'].split(),
504 native: false, language: ['c', 'cpp', 'objc'])
505 glib = declare_dependency(compile_args: config_host['GLIB_CFLAGS'].split(),
506 link_args: config_host['GLIB_LIBS'].split(),
507 version: config_host['GLIB_VERSION'],
509 'bindir': config_host['GLIB_BINDIR'],
511 # override glib dep with the configure results (for subprojects)
512 meson.override_dependency('glib-2.0', glib)
515 gdbus_codegen = not_found
516 gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio'
517 if not get_option('gio').auto() or have_system
518 gio = dependency('gio-2.0', required: get_option('gio'),
519 method: 'pkg-config', kwargs: static_kwargs)
520 if gio.found() and not cc.links('''
524 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
526 }''', dependencies: [glib, gio])
527 if get_option('gio').enabled()
528 error('The installed libgio is broken for static linking')
533 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'),
534 required: get_option('gio'))
535 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'),
536 method: 'pkg-config', kwargs: static_kwargs)
537 gio = declare_dependency(dependencies: [gio, gio_unix],
538 version: gio.version())
541 if gdbus_codegen.found() and get_option('cfi')
542 gdbus_codegen = not_found
543 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity'
547 if 'ust' in get_option('trace_backends')
548 lttng = dependency('lttng-ust', required: true, version: '>= 2.1',
549 method: 'pkg-config', kwargs: static_kwargs)
552 if have_system or have_tools
553 pixman = dependency('pixman-1', required: have_system, version:'>=0.21.8',
554 method: 'pkg-config', kwargs: static_kwargs)
556 zlib = dependency('zlib', required: true, kwargs: static_kwargs)
559 if not get_option('linux_aio').auto() or have_block
560 libaio = cc.find_library('aio', has_headers: ['libaio.h'],
561 required: get_option('linux_aio'),
562 kwargs: static_kwargs)
565 linux_io_uring_test = '''
566 #include <liburing.h>
567 #include <linux/errqueue.h>
569 int main(void) { return 0; }'''
571 linux_io_uring = not_found
572 if not get_option('linux_io_uring').auto() or have_block
573 linux_io_uring = dependency('liburing', version: '>=0.3',
574 required: get_option('linux_io_uring'),
575 method: 'pkg-config', kwargs: static_kwargs)
576 if not cc.links(linux_io_uring_test)
577 linux_io_uring = not_found
582 if not get_option('libnfs').auto() or have_block
583 libnfs = dependency('libnfs', version: '>=1.9.3',
584 required: get_option('libnfs'),
585 method: 'pkg-config', kwargs: static_kwargs)
590 #include <sys/types.h>
591 #ifdef CONFIG_LIBATTR
592 #include <attr/xattr.h>
594 #include <sys/xattr.h>
596 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }'''
599 have_old_libattr = false
600 if get_option('attr').allowed()
601 if cc.links(libattr_test)
602 libattr = declare_dependency()
604 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'],
605 required: get_option('attr'),
606 kwargs: static_kwargs)
607 if libattr.found() and not \
608 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR')
610 if get_option('attr').enabled()
611 error('could not link libattr')
613 warning('could not link libattr, disabling')
616 have_old_libattr = libattr.found()
621 cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'],
622 required: get_option('cocoa'))
624 vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet'))
625 if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h',
626 'VMNET_BRIDGED_MODE',
629 if get_option('vmnet').enabled()
630 error('vmnet.framework API is outdated')
632 warning('vmnet.framework API is outdated, disabling')
637 seccomp_has_sysrawrc = false
638 if not get_option('seccomp').auto() or have_system or have_tools
639 seccomp = dependency('libseccomp', version: '>=2.3.0',
640 required: get_option('seccomp'),
641 method: 'pkg-config', kwargs: static_kwargs)
643 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h',
644 'SCMP_FLTATR_API_SYSRAWRC',
645 dependencies: seccomp)
649 libcap_ng = not_found
650 if not get_option('cap_ng').auto() or have_system or have_tools
651 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'],
652 required: get_option('cap_ng'),
653 kwargs: static_kwargs)
655 if libcap_ng.found() and not cc.links('''
659 capng_capability_to_name(CAPNG_EFFECTIVE);
661 }''', dependencies: libcap_ng)
662 libcap_ng = not_found
663 if get_option('cap_ng').enabled()
664 error('could not link libcap-ng')
666 warning('could not link libcap-ng, disabling')
670 if get_option('xkbcommon').auto() and not have_system and not have_tools
671 xkbcommon = not_found
673 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'),
674 method: 'pkg-config', kwargs: static_kwargs)
678 if not get_option('slirp').auto() or have_system
679 slirp = dependency('slirp', required: get_option('slirp'),
680 method: 'pkg-config', kwargs: static_kwargs)
681 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because
682 # it passes function pointers within libslirp as callbacks for timers.
683 # When using a system-wide shared libslirp, the type information for the
684 # callback is missing and the timer call produces a false positive with CFI.
685 # Do not use the "version" keyword argument to produce a better error.
686 # with control-flow integrity.
687 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7')
688 if get_option('slirp').enabled()
689 error('Control-Flow Integrity requires libslirp 4.7.')
691 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.')
698 if not get_option('vde').auto() or have_system or have_tools
699 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'],
700 required: get_option('vde'),
701 kwargs: static_kwargs)
703 if vde.found() and not cc.links('''
704 #include <libvdeplug.h>
707 struct vde_open_args a = {0, 0, 0};
711 }''', dependencies: vde)
713 if get_option('cap_ng').enabled()
714 error('could not link libvdeplug')
716 warning('could not link libvdeplug, disabling')
721 if not get_option('pa').auto() or (targetos == 'linux' and have_system)
722 pulse = dependency('libpulse', required: get_option('pa'),
723 method: 'pkg-config', kwargs: static_kwargs)
726 if not get_option('alsa').auto() or (targetos == 'linux' and have_system)
727 alsa = dependency('alsa', required: get_option('alsa'),
728 method: 'pkg-config', kwargs: static_kwargs)
731 if not get_option('jack').auto() or have_system
732 jack = dependency('jack', required: get_option('jack'),
733 method: 'pkg-config', kwargs: static_kwargs)
736 if not get_option('sndio').auto() or have_system
737 sndio = dependency('sndio', required: get_option('sndio'),
738 method: 'pkg-config', kwargs: static_kwargs)
741 spice_protocol = not_found
742 if not get_option('spice_protocol').auto() or have_system
743 spice_protocol = dependency('spice-protocol', version: '>=0.12.3',
744 required: get_option('spice_protocol'),
745 method: 'pkg-config', kwargs: static_kwargs)
748 if not get_option('spice').auto() or have_system
749 spice = dependency('spice-server', version: '>=0.12.5',
750 required: get_option('spice'),
751 method: 'pkg-config', kwargs: static_kwargs)
753 spice_headers = spice.partial_dependency(compile_args: true, includes: true)
755 rt = cc.find_library('rt', required: false)
758 if not get_option('libiscsi').auto() or have_block
759 libiscsi = dependency('libiscsi', version: '>=1.9.0',
760 required: get_option('libiscsi'),
761 method: 'pkg-config', kwargs: static_kwargs)
764 if not get_option('zstd').auto() or have_block
765 zstd = dependency('libzstd', version: '>=1.4.0',
766 required: get_option('zstd'),
767 method: 'pkg-config', kwargs: static_kwargs)
771 have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found()
772 if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu
773 virgl = dependency('virglrenderer',
774 method: 'pkg-config',
775 required: get_option('virglrenderer'),
776 kwargs: static_kwargs)
779 if not get_option('blkio').auto() or have_block
780 blkio = dependency('blkio',
781 method: 'pkg-config',
782 required: get_option('blkio'),
783 kwargs: static_kwargs)
786 if not get_option('curl').auto() or have_block
787 curl = dependency('libcurl', version: '>=7.29.0',
788 method: 'pkg-config',
789 required: get_option('curl'),
790 kwargs: static_kwargs)
793 if targetos == 'linux' and (have_system or have_tools)
794 libudev = dependency('libudev',
795 method: 'pkg-config',
796 required: get_option('libudev'),
797 kwargs: static_kwargs)
800 mpathlibs = [libudev]
801 mpathpersist = not_found
802 mpathpersist_new_api = false
803 if targetos == 'linux' and have_tools and get_option('mpath').allowed()
804 mpath_test_source_new = '''
806 #include <mpath_persist.h>
807 unsigned mpath_mx_alloc_len = 1024;
809 static struct config *multipath_conf;
810 extern struct udev *udev;
811 extern struct config *get_multipath_config(void);
812 extern void put_multipath_config(struct config *conf);
814 struct config *get_multipath_config(void) { return multipath_conf; }
815 void put_multipath_config(struct config *conf) { }
818 multipath_conf = mpath_lib_init();
821 mpath_test_source_old = '''
823 #include <mpath_persist.h>
824 unsigned mpath_mx_alloc_len = 1024;
827 struct udev *udev = udev_new();
828 mpath_lib_init(udev);
831 libmpathpersist = cc.find_library('mpathpersist',
832 required: get_option('mpath'),
833 kwargs: static_kwargs)
834 if libmpathpersist.found()
835 mpathlibs += libmpathpersist
837 mpathlibs += cc.find_library('devmapper',
838 required: get_option('mpath'),
839 kwargs: static_kwargs)
841 mpathlibs += cc.find_library('multipath',
842 required: get_option('mpath'),
843 kwargs: static_kwargs)
844 foreach lib: mpathlibs
850 if mpathlibs.length() == 0
851 msg = 'Dependencies missing for libmpathpersist'
852 elif cc.links(mpath_test_source_new, dependencies: mpathlibs)
853 mpathpersist = declare_dependency(dependencies: mpathlibs)
854 mpathpersist_new_api = true
855 elif cc.links(mpath_test_source_old, dependencies: mpathlibs)
856 mpathpersist = declare_dependency(dependencies: mpathlibs)
858 msg = 'Cannot detect libmpathpersist API'
860 if not mpathpersist.found()
861 if get_option('mpath').enabled()
864 warning(msg + ', disabling')
872 if have_system and get_option('curses').allowed()
874 #if defined(__APPLE__) || defined(__OpenBSD__)
875 #define _XOPEN_SOURCE_EXTENDED 1
882 setlocale(LC_ALL, "");
884 addwstr(L"wide chars\n");
886 add_wch(WACS_DEGREE);
890 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw']
891 curses = dependency(curses_dep_list,
893 method: 'pkg-config',
894 kwargs: static_kwargs)
895 msg = get_option('curses').enabled() ? 'curses library not found' : ''
896 curses_compile_args = ['-DNCURSES_WIDECHAR=1']
898 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses])
899 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses])
901 msg = 'curses package not usable'
905 if not curses.found()
906 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
907 if targetos != 'windows' and not has_curses_h
908 message('Trying with /usr/include/ncursesw')
909 curses_compile_args += ['-I/usr/include/ncursesw']
910 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
913 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw'])
914 foreach curses_libname : curses_libname_list
915 libcurses = cc.find_library(curses_libname,
917 kwargs: static_kwargs)
919 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses)
920 curses = declare_dependency(compile_args: curses_compile_args,
921 dependencies: [libcurses])
924 msg = 'curses library not usable'
930 if get_option('iconv').allowed()
931 foreach link_args : [ ['-liconv'], [] ]
932 # Programs will be linked with glib and this will bring in libiconv on FreeBSD.
933 # We need to use libiconv if available because mixing libiconv's headers with
934 # the system libc does not work.
935 # However, without adding glib to the dependencies -L/usr/local/lib will not be
936 # included in the command line and libiconv will not be found.
940 iconv_t conv = iconv_open("WCHAR_T", "UCS-2");
941 return conv != (iconv_t) -1;
942 }''', args: config_host['GLIB_CFLAGS'].split() + config_host['GLIB_LIBS'].split() + link_args)
943 iconv = declare_dependency(link_args: link_args, dependencies: glib)
948 if curses.found() and not iconv.found()
949 if get_option('iconv').enabled()
950 error('iconv not available')
952 msg = 'iconv required for curses UI but not available'
955 if not curses.found() and msg != ''
956 if get_option('curses').enabled()
959 warning(msg + ', disabling')
965 if not get_option('brlapi').auto() or have_system
966 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'],
967 required: get_option('brlapi'),
968 kwargs: static_kwargs)
969 if brlapi.found() and not cc.links('''
972 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi)
974 if get_option('brlapi').enabled()
975 error('could not link brlapi')
977 warning('could not link brlapi, disabling')
983 if not get_option('sdl').auto() or have_system
984 sdl = dependency('sdl2', required: get_option('sdl'), kwargs: static_kwargs)
985 sdl_image = not_found
988 # work around 2.0.8 bug
989 sdl = declare_dependency(compile_args: '-Wno-undef',
991 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'),
992 method: 'pkg-config', kwargs: static_kwargs)
994 if get_option('sdl_image').enabled()
995 error('sdl-image required, but SDL was @0@'.format(
996 get_option('sdl').disabled() ? 'disabled' : 'not found'))
998 sdl_image = not_found
1002 if not get_option('rbd').auto() or have_block
1003 librados = cc.find_library('rados', required: get_option('rbd'),
1004 kwargs: static_kwargs)
1005 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'],
1006 required: get_option('rbd'),
1007 kwargs: static_kwargs)
1008 if librados.found() and librbd.found()
1011 #include <rbd/librbd.h>
1014 rados_create(&cluster, NULL);
1015 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0)
1019 }''', dependencies: [librbd, librados])
1020 rbd = declare_dependency(dependencies: [librbd, librados])
1021 elif get_option('rbd').enabled()
1022 error('librbd >= 1.12.0 required')
1024 warning('librbd >= 1.12.0 not found, disabling')
1029 glusterfs = not_found
1030 glusterfs_ftruncate_has_stat = false
1031 glusterfs_iocb_has_stat = false
1032 if not get_option('glusterfs').auto() or have_block
1033 glusterfs = dependency('glusterfs-api', version: '>=3',
1034 required: get_option('glusterfs'),
1035 method: 'pkg-config', kwargs: static_kwargs)
1036 if glusterfs.found()
1037 glusterfs_ftruncate_has_stat = cc.links('''
1038 #include <glusterfs/api/glfs.h>
1043 /* new glfs_ftruncate() passes two additional args */
1044 return glfs_ftruncate(NULL, 0, NULL, NULL);
1046 ''', dependencies: glusterfs)
1047 glusterfs_iocb_has_stat = cc.links('''
1048 #include <glusterfs/api/glfs.h>
1050 /* new glfs_io_cbk() passes two additional glfs_stat structs */
1052 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
1058 glfs_io_cbk iocb = &glusterfs_iocb;
1059 iocb(NULL, 0 , NULL, NULL, NULL);
1062 ''', dependencies: glusterfs)
1067 if not get_option('libssh').auto() or have_block
1068 libssh = dependency('libssh', version: '>=0.8.7',
1069 method: 'pkg-config',
1070 required: get_option('libssh'),
1071 kwargs: static_kwargs)
1074 libbzip2 = not_found
1075 if not get_option('bzip2').auto() or have_block
1076 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'],
1077 required: get_option('bzip2'),
1078 kwargs: static_kwargs)
1079 if libbzip2.found() and not cc.links('''
1081 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2)
1082 libbzip2 = not_found
1083 if get_option('bzip2').enabled()
1084 error('could not link libbzip2')
1086 warning('could not link libbzip2, disabling')
1091 liblzfse = not_found
1092 if not get_option('lzfse').auto() or have_block
1093 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'],
1094 required: get_option('lzfse'),
1095 kwargs: static_kwargs)
1097 if liblzfse.found() and not cc.links('''
1099 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse)
1100 liblzfse = not_found
1101 if get_option('lzfse').enabled()
1102 error('could not link liblzfse')
1104 warning('could not link liblzfse, disabling')
1109 if get_option('oss').allowed() and have_system
1110 if not cc.has_header('sys/soundcard.h')
1112 elif targetos == 'netbsd'
1113 oss = cc.find_library('ossaudio', required: get_option('oss'),
1114 kwargs: static_kwargs)
1116 oss = declare_dependency()
1120 if get_option('oss').enabled()
1121 error('OSS not found')
1126 if not get_option('dsound').auto() or (targetos == 'windows' and have_system)
1127 if cc.has_header('dsound.h')
1128 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid'])
1131 if not dsound.found()
1132 if get_option('dsound').enabled()
1133 error('DirectSound not found')
1138 coreaudio = not_found
1139 if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system)
1140 coreaudio = dependency('appleframeworks', modules: 'CoreAudio',
1141 required: get_option('coreaudio'))
1145 if not get_option('opengl').auto() or have_system or have_vhost_user_gpu
1146 epoxy = dependency('epoxy', method: 'pkg-config',
1147 required: get_option('opengl'), kwargs: static_kwargs)
1148 if cc.has_header('epoxy/egl.h', dependencies: epoxy)
1150 elif get_option('opengl').enabled()
1151 error('epoxy/egl.h not found')
1155 if (have_system or have_tools) and (virgl.found() or opengl.found())
1156 gbm = dependency('gbm', method: 'pkg-config', required: false,
1157 kwargs: static_kwargs)
1159 have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found()
1162 gnutls_crypto = not_found
1163 if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system)
1164 # For general TLS support our min gnutls matches
1165 # that implied by our platform support matrix
1167 # For the crypto backends, we look for a newer
1170 # Version 3.6.8 is needed to get XTS
1171 # Version 3.6.13 is needed to get PBKDF
1172 # Version 3.6.14 is needed to get HW accelerated XTS
1174 # If newer enough gnutls isn't available, we can
1175 # still use a different crypto backend to satisfy
1176 # the platform support requirements
1177 gnutls_crypto = dependency('gnutls', version: '>=3.6.14',
1178 method: 'pkg-config',
1180 kwargs: static_kwargs)
1181 if gnutls_crypto.found()
1182 gnutls = gnutls_crypto
1184 # Our min version if all we need is TLS
1185 gnutls = dependency('gnutls', version: '>=3.5.18',
1186 method: 'pkg-config',
1187 required: get_option('gnutls'),
1188 kwargs: static_kwargs)
1192 # We prefer use of gnutls for crypto, unless the options
1193 # explicitly asked for nettle or gcrypt.
1195 # If gnutls isn't available for crypto, then we'll prefer
1196 # gcrypt over nettle for performance reasons.
1202 if get_option('nettle').enabled() and get_option('gcrypt').enabled()
1203 error('Only one of gcrypt & nettle can be enabled')
1206 # Explicit nettle/gcrypt request, so ignore gnutls for crypto
1207 if get_option('nettle').enabled() or get_option('gcrypt').enabled()
1208 gnutls_crypto = not_found
1211 if not gnutls_crypto.found()
1212 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled()
1213 gcrypt = dependency('libgcrypt', version: '>=1.8',
1214 method: 'config-tool',
1215 required: get_option('gcrypt'),
1216 kwargs: static_kwargs)
1217 # Debian has removed -lgpg-error from libgcrypt-config
1218 # as it "spreads unnecessary dependencies" which in
1219 # turn breaks static builds...
1220 if gcrypt.found() and enable_static
1221 gcrypt = declare_dependency(dependencies: [
1223 cc.find_library('gpg-error', required: true, kwargs: static_kwargs)])
1226 if (not get_option('nettle').auto() or have_system) and not gcrypt.found()
1227 nettle = dependency('nettle', version: '>=3.4',
1228 method: 'pkg-config',
1229 required: get_option('nettle'),
1230 kwargs: static_kwargs)
1231 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle)
1237 gmp = dependency('gmp', required: false, method: 'pkg-config', kwargs: static_kwargs)
1238 if nettle.found() and gmp.found()
1239 hogweed = dependency('hogweed', version: '>=3.4',
1240 method: 'pkg-config',
1241 required: get_option('nettle'),
1242 kwargs: static_kwargs)
1249 have_gtk_clipboard = get_option('gtk_clipboard').enabled()
1251 if not get_option('gtk').auto() or have_system
1252 gtk = dependency('gtk+-3.0', version: '>=3.22.0',
1253 method: 'pkg-config',
1254 required: get_option('gtk'),
1255 kwargs: static_kwargs)
1257 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0',
1258 method: 'pkg-config',
1260 kwargs: static_kwargs)
1261 gtk = declare_dependency(dependencies: [gtk, gtkx11])
1263 if not get_option('vte').auto() or have_system
1264 vte = dependency('vte-2.91',
1265 method: 'pkg-config',
1266 required: get_option('vte'),
1267 kwargs: static_kwargs)
1269 elif have_gtk_clipboard
1270 error('GTK clipboard requested, but GTK not found')
1276 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found(),
1277 kwargs: static_kwargs)
1280 if get_option('png').allowed() and have_system
1281 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'),
1282 method: 'pkg-config', kwargs: static_kwargs)
1287 if get_option('vnc').allowed() and have_system
1288 vnc = declare_dependency() # dummy dependency
1289 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'),
1290 method: 'pkg-config', kwargs: static_kwargs)
1291 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'],
1292 required: get_option('vnc_sasl'),
1293 kwargs: static_kwargs)
1295 sasl = declare_dependency(dependencies: sasl,
1296 compile_args: '-DSTRUCT_IOVEC_DEFINED')
1301 if not get_option('auth_pam').auto() or have_system
1302 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'],
1303 required: get_option('auth_pam'),
1304 kwargs: static_kwargs)
1306 if pam.found() and not cc.links('''
1308 #include <security/pam_appl.h>
1310 const char *service_name = "qemu";
1311 const char *user = "frank";
1312 const struct pam_conv pam_conv = { 0 };
1313 pam_handle_t *pamh = NULL;
1314 pam_start(service_name, user, &pam_conv, &pamh);
1316 }''', dependencies: pam)
1318 if get_option('auth_pam').enabled()
1319 error('could not link libpam')
1321 warning('could not link libpam, disabling')
1326 if not get_option('snappy').auto() or have_system
1327 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'],
1328 required: get_option('snappy'),
1329 kwargs: static_kwargs)
1331 if snappy.found() and not linker.links('''
1332 #include <snappy-c.h>
1333 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy)
1335 if get_option('snappy').enabled()
1336 error('could not link libsnappy')
1338 warning('could not link libsnappy, disabling')
1343 if not get_option('lzo').auto() or have_system
1344 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'],
1345 required: get_option('lzo'),
1346 kwargs: static_kwargs)
1348 if lzo.found() and not cc.links('''
1349 #include <lzo/lzo1x.h>
1350 int main(void) { lzo_version(); return 0; }''', dependencies: lzo)
1352 if get_option('lzo').enabled()
1353 error('could not link liblzo2')
1355 warning('could not link liblzo2, disabling')
1360 if not get_option('numa').auto() or have_system or have_tools
1361 numa = cc.find_library('numa', has_headers: ['numa.h'],
1362 required: get_option('numa'),
1363 kwargs: static_kwargs)
1365 if numa.found() and not cc.links('''
1367 int main(void) { return numa_available(); }
1368 ''', dependencies: numa)
1370 if get_option('numa').enabled()
1371 error('could not link numa')
1373 warning('could not link numa, disabling')
1378 if not get_option('rdma').auto() or have_system
1379 libumad = cc.find_library('ibumad', required: get_option('rdma'))
1380 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'],
1381 required: get_option('rdma'),
1382 kwargs: static_kwargs),
1383 cc.find_library('ibverbs', required: get_option('rdma'),
1384 kwargs: static_kwargs),
1386 rdma = declare_dependency(dependencies: rdma_libs)
1387 foreach lib: rdma_libs
1395 if get_option('xen').enabled() or (get_option('xen').auto() and have_system)
1396 xencontrol = dependency('xencontrol', required: false,
1397 method: 'pkg-config', kwargs: static_kwargs)
1398 if xencontrol.found()
1399 xen_pc = declare_dependency(version: xencontrol.version(),
1402 # disabler: true makes xen_pc.found() return false if any is not found
1403 dependency('xenstore', required: false,
1404 method: 'pkg-config', kwargs: static_kwargs,
1406 dependency('xenforeignmemory', required: false,
1407 method: 'pkg-config', kwargs: static_kwargs,
1409 dependency('xengnttab', required: false,
1410 method: 'pkg-config', kwargs: static_kwargs,
1412 dependency('xenevtchn', required: false,
1413 method: 'pkg-config', kwargs: static_kwargs,
1415 dependency('xendevicemodel', required: false,
1416 method: 'pkg-config', kwargs: static_kwargs,
1418 # optional, no "disabler: true"
1419 dependency('xentoolcore', required: false,
1420 method: 'pkg-config', kwargs: static_kwargs)])
1426 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' ]
1428 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1429 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1430 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1431 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1432 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1433 '4.6.0': [ 'xenstore', 'xenctrl' ],
1434 '4.5.0': [ 'xenstore', 'xenctrl' ],
1435 '4.2.0': [ 'xenstore', 'xenctrl' ],
1438 foreach ver: xen_tests
1439 # cache the various library tests to avoid polluting the logs
1441 foreach l: xen_libs[ver]
1442 if l not in xen_deps
1443 xen_deps += { l: cc.find_library(l, required: false) }
1445 xen_test_deps += xen_deps[l]
1448 # Use -D to pick just one of the test programs in scripts/xen-detect.c
1449 xen_version = ver.split('.')
1450 xen_ctrl_version = xen_version[0] + \
1451 ('0' + xen_version[1]).substring(-2) + \
1452 ('0' + xen_version[2]).substring(-2)
1453 if cc.links(files('scripts/xen-detect.c'),
1454 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version,
1455 dependencies: xen_test_deps)
1456 xen = declare_dependency(version: ver, dependencies: xen_test_deps)
1462 accelerators += 'CONFIG_XEN'
1463 elif get_option('xen').enabled()
1464 error('could not compile and link Xen test program')
1467 have_xen_pci_passthrough = get_option('xen_pci_passthrough') \
1468 .require(xen.found(),
1469 error_message: 'Xen PCI passthrough requested but Xen not enabled') \
1470 .require(targetos == 'linux',
1471 error_message: 'Xen PCI passthrough not available on this platform') \
1476 if not get_option('smartcard').auto() or have_system
1477 cacard = dependency('libcacard', required: get_option('smartcard'),
1478 version: '>=2.5.1', method: 'pkg-config',
1479 kwargs: static_kwargs)
1483 u2f = dependency('u2f-emu', required: get_option('u2f'),
1484 method: 'pkg-config',
1485 kwargs: static_kwargs)
1489 canokey = dependency('canokey-qemu', required: get_option('canokey'),
1490 method: 'pkg-config',
1491 kwargs: static_kwargs)
1493 usbredir = not_found
1494 if not get_option('usb_redir').auto() or have_system
1495 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'),
1496 version: '>=0.6', method: 'pkg-config',
1497 kwargs: static_kwargs)
1500 if not get_option('libusb').auto() or have_system
1501 libusb = dependency('libusb-1.0', required: get_option('libusb'),
1502 version: '>=1.0.13', method: 'pkg-config',
1503 kwargs: static_kwargs)
1507 if not get_option('libpmem').auto() or have_system
1508 libpmem = dependency('libpmem', required: get_option('libpmem'),
1509 method: 'pkg-config', kwargs: static_kwargs)
1511 libdaxctl = not_found
1512 if not get_option('libdaxctl').auto() or have_system
1513 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'),
1514 version: '>=57', method: 'pkg-config',
1515 kwargs: static_kwargs)
1519 tasn1 = dependency('libtasn1',
1520 method: 'pkg-config',
1521 kwargs: static_kwargs)
1523 keyutils = dependency('libkeyutils', required: false,
1524 method: 'pkg-config', kwargs: static_kwargs)
1526 has_gettid = cc.has_function('gettid')
1529 selinux = dependency('libselinux',
1530 required: get_option('selinux'),
1531 method: 'pkg-config', kwargs: static_kwargs)
1536 if get_option('malloc') == 'system'
1538 get_option('malloc_trim').allowed() and \
1539 cc.links('''#include <malloc.h>
1540 int main(void) { malloc_trim(0); return 0; }''')
1542 has_malloc_trim = false
1543 malloc = cc.find_library(get_option('malloc'), required: true)
1545 if not has_malloc_trim and get_option('malloc_trim').enabled()
1546 if get_option('malloc') == 'system'
1547 error('malloc_trim not available on this platform.')
1549 error('malloc_trim not available with non-libc memory allocator')
1553 # Check whether the glibc provides statx()
1555 gnu_source_prefix = '''
1560 statx_test = gnu_source_prefix + '''
1561 #include <sys/stat.h>
1563 struct statx statxbuf;
1564 statx(0, "", 0, STATX_BASIC_STATS, &statxbuf);
1568 has_statx = cc.links(statx_test)
1570 # Check whether statx() provides mount ID information
1572 statx_mnt_id_test = gnu_source_prefix + '''
1573 #include <sys/stat.h>
1575 struct statx statxbuf;
1576 statx(0, "", 0, STATX_BASIC_STATS | STATX_MNT_ID, &statxbuf);
1577 return statxbuf.stx_mnt_id;
1580 has_statx_mnt_id = cc.links(statx_mnt_id_test)
1582 have_vhost_user_blk_server = get_option('vhost_user_blk_server') \
1583 .require(targetos == 'linux',
1584 error_message: 'vhost_user_blk_server requires linux') \
1585 .require(have_vhost_user,
1586 error_message: 'vhost_user_blk_server requires vhost-user support') \
1587 .disable_auto_if(not have_tools and not have_system) \
1590 if get_option('fuse').disabled() and get_option('fuse_lseek').enabled()
1591 error('Cannot enable fuse-lseek while fuse is disabled')
1594 fuse = dependency('fuse3', required: get_option('fuse'),
1595 version: '>=3.1', method: 'pkg-config',
1596 kwargs: static_kwargs)
1598 fuse_lseek = not_found
1599 if get_option('fuse_lseek').allowed()
1600 if fuse.version().version_compare('>=3.8')
1602 fuse_lseek = declare_dependency()
1603 elif get_option('fuse_lseek').enabled()
1605 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version())
1607 error('fuse-lseek requires libfuse, which was not found')
1612 have_libvduse = (targetos == 'linux')
1613 if get_option('libvduse').enabled()
1614 if targetos != 'linux'
1615 error('libvduse requires linux')
1617 elif get_option('libvduse').disabled()
1618 have_libvduse = false
1621 have_vduse_blk_export = (have_libvduse and targetos == 'linux')
1622 if get_option('vduse_blk_export').enabled()
1623 if targetos != 'linux'
1624 error('vduse_blk_export requires linux')
1625 elif not have_libvduse
1626 error('vduse_blk_export requires libvduse support')
1628 elif get_option('vduse_blk_export').disabled()
1629 have_vduse_blk_export = false
1633 libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config')
1634 if libbpf.found() and not cc.links('''
1635 #include <bpf/libbpf.h>
1638 bpf_object__destroy_skeleton(NULL);
1640 }''', dependencies: libbpf)
1642 if get_option('bpf').enabled()
1643 error('libbpf skeleton test failed')
1645 warning('libbpf skeleton test failed, disabling')
1653 audio_drivers_selected = []
1655 audio_drivers_available = {
1656 'alsa': alsa.found(),
1657 'coreaudio': coreaudio.found(),
1658 'dsound': dsound.found(),
1659 'jack': jack.found(),
1661 'pa': pulse.found(),
1663 'sndio': sndio.found(),
1665 foreach k, v: audio_drivers_available
1666 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v)
1669 # Default to native drivers first, OSS second, SDL third
1670 audio_drivers_priority = \
1671 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \
1672 (targetos == 'linux' ? [] : [ 'sdl' ])
1673 audio_drivers_default = []
1674 foreach k: audio_drivers_priority
1675 if audio_drivers_available[k]
1676 audio_drivers_default += k
1680 foreach k: get_option('audio_drv_list')
1682 audio_drivers_selected += audio_drivers_default
1683 elif not audio_drivers_available[k]
1684 error('Audio driver "@0@" not available.'.format(k))
1686 audio_drivers_selected += k
1690 config_host_data.set('CONFIG_AUDIO_DRIVERS',
1691 '"' + '", "'.join(audio_drivers_selected) + '", ')
1693 if get_option('cfi')
1695 # Check for dependency on LTO
1696 if not get_option('b_lto')
1697 error('Selected Control-Flow Integrity but LTO is disabled')
1699 if config_host.has_key('CONFIG_MODULES')
1700 error('Selected Control-Flow Integrity is not compatible with modules')
1702 # Check for cfi flags. CFI requires LTO so we can't use
1703 # get_supported_arguments, but need a more complex "compiles" which allows
1705 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall',
1706 args: ['-flto', '-fsanitize=cfi-icall'] )
1707 cfi_flags += '-fsanitize=cfi-icall'
1709 error('-fsanitize=cfi-icall is not supported by the compiler')
1711 if cc.compiles('int main () { return 0; }',
1712 name: '-fsanitize-cfi-icall-generalize-pointers',
1713 args: ['-flto', '-fsanitize=cfi-icall',
1714 '-fsanitize-cfi-icall-generalize-pointers'] )
1715 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers'
1717 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler')
1719 if get_option('cfi_debug')
1720 if cc.compiles('int main () { return 0; }',
1721 name: '-fno-sanitize-trap=cfi-icall',
1722 args: ['-flto', '-fsanitize=cfi-icall',
1723 '-fno-sanitize-trap=cfi-icall'] )
1724 cfi_flags += '-fno-sanitize-trap=cfi-icall'
1726 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler')
1729 add_global_arguments(cfi_flags, native: false, language: ['c', 'cpp', 'objc'])
1730 add_global_link_arguments(cfi_flags, native: false, language: ['c', 'cpp', 'objc'])
1733 have_host_block_device = (targetos != 'darwin' or
1734 cc.has_header('IOKit/storage/IOMedia.h'))
1736 dbus_display = get_option('dbus_display') \
1737 .require(gio.version().version_compare('>=2.64'),
1738 error_message: '-display dbus requires glib>=2.64') \
1739 .require(gdbus_codegen.found(),
1740 error_message: gdbus_codegen_error.format('-display dbus')) \
1741 .require(opengl.found() and gbm.found(),
1742 error_message: '-display dbus requires epoxy/egl and gbm') \
1745 have_virtfs = get_option('virtfs') \
1746 .require(targetos == 'linux' or targetos == 'darwin',
1747 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \
1748 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'),
1749 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \
1750 .require(targetos == 'darwin' or (libattr.found() and libcap_ng.found()),
1751 error_message: 'virtio-9p (virtfs) on Linux requires libcap-ng-devel and libattr-devel') \
1752 .disable_auto_if(not have_tools and not have_system) \
1755 have_virtfs_proxy_helper = targetos != 'darwin' and have_virtfs and have_tools
1757 if get_option('block_drv_ro_whitelist') == ''
1758 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '')
1760 config_host_data.set('CONFIG_BDRV_RO_WHITELIST',
1761 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ')
1763 if get_option('block_drv_rw_whitelist') == ''
1764 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '')
1766 config_host_data.set('CONFIG_BDRV_RW_WHITELIST',
1767 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ')
1770 foreach k : get_option('trace_backends')
1771 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true)
1773 config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file'))
1774 config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority'))
1776 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path())
1778 config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir'))
1779 config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix'))
1780 config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir)
1781 config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir)
1782 config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir)
1784 qemu_firmwarepath = ''
1785 foreach k : get_option('qemu_firmwarepath')
1786 qemu_firmwarepath += '"' + get_option('prefix') / k + '", '
1788 config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath)
1790 config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir'))
1791 config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir)
1792 config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir'))
1793 config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir'))
1794 config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir)
1795 config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir'))
1797 if config_host.has_key('CONFIG_MODULES')
1798 config_host_data.set('CONFIG_STAMP', run_command(
1799 meson.current_source_dir() / 'scripts/qemu-stamp.py',
1800 meson.project_version(), get_option('pkgversion'), '--',
1801 meson.current_source_dir() / 'configure',
1802 capture: true, check: true).stdout().strip())
1805 have_slirp_smbd = get_option('slirp_smbd') \
1806 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \
1809 smbd_path = get_option('smbd')
1811 smbd_path = (targetos == 'solaris' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd')
1813 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path)
1816 config_host_data.set('HOST_' + host_arch.to_upper(), 1)
1818 if get_option('module_upgrades') and not enable_modules
1819 error('Cannot enable module-upgrades as modules are not enabled')
1821 config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades'))
1823 config_host_data.set('CONFIG_ATTR', libattr.found())
1824 config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools'))
1825 config_host_data.set('CONFIG_BRLAPI', brlapi.found())
1826 config_host_data.set('CONFIG_COCOA', cocoa.found())
1827 config_host_data.set('CONFIG_FUZZ', get_option('fuzzing'))
1828 config_host_data.set('CONFIG_GCOV', get_option('b_coverage'))
1829 config_host_data.set('CONFIG_LIBUDEV', libudev.found())
1830 config_host_data.set('CONFIG_LZO', lzo.found())
1831 config_host_data.set('CONFIG_MPATH', mpathpersist.found())
1832 config_host_data.set('CONFIG_MPATH_NEW_API', mpathpersist_new_api)
1833 config_host_data.set('CONFIG_BLKIO', blkio.found())
1834 config_host_data.set('CONFIG_CURL', curl.found())
1835 config_host_data.set('CONFIG_CURSES', curses.found())
1836 config_host_data.set('CONFIG_GBM', gbm.found())
1837 config_host_data.set('CONFIG_GIO', gio.found())
1838 config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found())
1839 if glusterfs.found()
1840 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4'))
1841 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5'))
1842 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6'))
1843 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6'))
1844 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat)
1845 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat)
1847 config_host_data.set('CONFIG_GTK', gtk.found())
1848 config_host_data.set('CONFIG_VTE', vte.found())
1849 config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard)
1850 config_host_data.set('CONFIG_LIBATTR', have_old_libattr)
1851 config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found())
1852 config_host_data.set('CONFIG_EBPF', libbpf.found())
1853 config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found())
1854 config_host_data.set('CONFIG_LIBISCSI', libiscsi.found())
1855 config_host_data.set('CONFIG_LIBNFS', libnfs.found())
1856 config_host_data.set('CONFIG_LIBSSH', libssh.found())
1857 config_host_data.set('CONFIG_LINUX_AIO', libaio.found())
1858 config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found())
1859 config_host_data.set('CONFIG_LIBPMEM', libpmem.found())
1860 config_host_data.set('CONFIG_NUMA', numa.found())
1861 config_host_data.set('CONFIG_OPENGL', opengl.found())
1862 config_host_data.set('CONFIG_PROFILER', get_option('profiler'))
1863 config_host_data.set('CONFIG_RBD', rbd.found())
1864 config_host_data.set('CONFIG_RDMA', rdma.found())
1865 config_host_data.set('CONFIG_SDL', sdl.found())
1866 config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found())
1867 config_host_data.set('CONFIG_SECCOMP', seccomp.found())
1869 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc)
1871 config_host_data.set('CONFIG_SNAPPY', snappy.found())
1872 config_host_data.set('CONFIG_TPM', have_tpm)
1873 config_host_data.set('CONFIG_USB_LIBUSB', libusb.found())
1874 config_host_data.set('CONFIG_VDE', vde.found())
1875 config_host_data.set('CONFIG_VHOST_NET', have_vhost_net)
1876 config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user)
1877 config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa)
1878 config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel)
1879 config_host_data.set('CONFIG_VHOST_USER', have_vhost_user)
1880 config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto)
1881 config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa)
1882 config_host_data.set('CONFIG_VMNET', vmnet.found())
1883 config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server)
1884 config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export)
1885 config_host_data.set('CONFIG_PNG', png.found())
1886 config_host_data.set('CONFIG_VNC', vnc.found())
1887 config_host_data.set('CONFIG_VNC_JPEG', jpeg.found())
1888 config_host_data.set('CONFIG_VNC_SASL', sasl.found())
1889 config_host_data.set('CONFIG_VIRTFS', have_virtfs)
1890 config_host_data.set('CONFIG_VTE', vte.found())
1891 config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found())
1892 config_host_data.set('CONFIG_KEYUTILS', keyutils.found())
1893 config_host_data.set('CONFIG_GETTID', has_gettid)
1894 config_host_data.set('CONFIG_GNUTLS', gnutls.found())
1895 config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found())
1896 config_host_data.set('CONFIG_TASN1', tasn1.found())
1897 config_host_data.set('CONFIG_GCRYPT', gcrypt.found())
1898 config_host_data.set('CONFIG_NETTLE', nettle.found())
1899 config_host_data.set('CONFIG_HOGWEED', hogweed.found())
1900 config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private')
1901 config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim)
1902 config_host_data.set('CONFIG_STATX', has_statx)
1903 config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id)
1904 config_host_data.set('CONFIG_ZSTD', zstd.found())
1905 config_host_data.set('CONFIG_FUSE', fuse.found())
1906 config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found())
1907 config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found())
1908 if spice_protocol.found()
1909 config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0])
1910 config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1])
1911 config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2])
1913 config_host_data.set('CONFIG_SPICE', spice.found())
1914 config_host_data.set('CONFIG_X11', x11.found())
1915 config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display)
1916 config_host_data.set('CONFIG_CFI', get_option('cfi'))
1917 config_host_data.set('CONFIG_SELINUX', selinux.found())
1918 config_host_data.set('CONFIG_XEN_BACKEND', xen.found())
1920 # protect from xen.version() having less than three components
1921 xen_version = xen.version().split('.') + ['0', '0']
1922 xen_ctrl_version = xen_version[0] + \
1923 ('0' + xen_version[1]).substring(-2) + \
1924 ('0' + xen_version[2]).substring(-2)
1925 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version)
1927 config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version()))
1928 config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0])
1929 config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1])
1930 config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2])
1932 config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf)
1933 config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device)
1935 have_coroutine_pool = get_option('coroutine_pool')
1936 if get_option('debug_stack_usage') and have_coroutine_pool
1937 message('Disabling coroutine pool to measure stack usage')
1938 have_coroutine_pool = false
1940 config_host_data.set10('CONFIG_COROUTINE_POOL', have_coroutine_pool)
1941 config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex'))
1942 config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage'))
1943 config_host_data.set('CONFIG_GPROF', get_option('gprof'))
1944 config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed())
1945 config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug'))
1946 config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed())
1949 config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h'))
1950 config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h'))
1951 config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h'))
1952 config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h'))
1953 config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h'))
1954 config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h'))
1955 config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h'))
1956 config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h'))
1957 config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h'))
1958 if targetos == 'windows'
1959 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h'))
1963 config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range'))
1964 config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4'))
1965 config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime'))
1966 config_host_data.set('CONFIG_DUP3', cc.has_function('dup3'))
1967 config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate'))
1968 config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate'))
1969 # Note that we need to specify prefix: here to avoid incorrectly
1970 # thinking that Windows has posix_memalign()
1971 config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>'))
1972 config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc'))
1973 config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc'))
1974 config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign'))
1975 config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll'))
1976 config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>'))
1977 config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np'))
1978 config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile'))
1979 config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare'))
1980 config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs'))
1981 config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range'))
1982 config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create'))
1983 config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range'))
1984 config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs'))
1985 config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util))
1986 config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul'))
1987 config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>'))
1989 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS',
1990 cc.has_function('rbd_namespace_exists',
1992 prefix: '#include <rbd/librbd.h>'))
1995 config_host_data.set('HAVE_IBV_ADVISE_MR',
1996 cc.has_function('ibv_advise_mr',
1998 prefix: '#include <infiniband/verbs.h>'))
2002 config_host_data.set('CONFIG_BYTESWAP_H',
2003 cc.has_header_symbol('byteswap.h', 'bswap_32'))
2004 config_host_data.set('CONFIG_EPOLL_CREATE1',
2005 cc.has_header_symbol('sys/epoll.h', 'epoll_create1'))
2006 config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE',
2007 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and
2008 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE'))
2009 config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE',
2010 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE'))
2011 config_host_data.set('CONFIG_FIEMAP',
2012 cc.has_header('linux/fiemap.h') and
2013 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP'))
2014 config_host_data.set('CONFIG_GETRANDOM',
2015 cc.has_function('getrandom') and
2016 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK'))
2017 config_host_data.set('CONFIG_INOTIFY',
2018 cc.has_header_symbol('sys/inotify.h', 'inotify_init'))
2019 config_host_data.set('CONFIG_INOTIFY1',
2020 cc.has_header_symbol('sys/inotify.h', 'inotify_init1'))
2021 config_host_data.set('CONFIG_MACHINE_BSWAP_H',
2022 cc.has_header_symbol('machine/bswap.h', 'bswap32',
2023 prefix: '''#include <sys/endian.h>
2024 #include <sys/types.h>'''))
2025 config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK',
2026 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK'))
2027 config_host_data.set('CONFIG_RTNETLINK',
2028 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN'))
2029 config_host_data.set('CONFIG_SYSMACROS',
2030 cc.has_header_symbol('sys/sysmacros.h', 'makedev'))
2031 config_host_data.set('HAVE_OPTRESET',
2032 cc.has_header_symbol('getopt.h', 'optreset'))
2033 config_host_data.set('HAVE_IPPROTO_MPTCP',
2034 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP'))
2037 config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID',
2038 cc.has_member('struct sigevent', 'sigev_notify_thread_id',
2039 prefix: '#include <signal.h>'))
2040 config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM',
2041 cc.has_member('struct stat', 'st_atim',
2042 prefix: '#include <sys/stat.h>'))
2045 config_host_data.set('CONFIG_IOVEC',
2046 cc.has_type('struct iovec',
2047 prefix: '#include <sys/uio.h>'))
2048 config_host_data.set('HAVE_UTMPX',
2049 cc.has_type('struct utmpx',
2050 prefix: '#include <utmpx.h>'))
2052 config_host_data.set('CONFIG_EVENTFD', cc.links('''
2053 #include <sys/eventfd.h>
2054 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }'''))
2055 config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + '''
2058 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
2059 return fdatasync(0);
2061 #error Not supported
2065 has_madvise = cc.links(gnu_source_prefix + '''
2066 #include <sys/types.h>
2067 #include <sys/mman.h>
2069 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''')
2070 missing_madvise_proto = false
2072 # Some platforms (illumos and Solaris before Solaris 11) provide madvise()
2073 # but forget to prototype it. In this case, has_madvise will be true (the
2074 # test program links despite a compile warning). To detect the
2075 # missing-prototype case, we try again with a definitely-bogus prototype.
2076 # This will only compile if the system headers don't provide the prototype;
2077 # otherwise the conflicting prototypes will cause a compiler error.
2078 missing_madvise_proto = cc.links(gnu_source_prefix + '''
2079 #include <sys/types.h>
2080 #include <sys/mman.h>
2082 extern int madvise(int);
2083 int main(void) { return madvise(0); }''')
2085 config_host_data.set('CONFIG_MADVISE', has_madvise)
2086 config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto)
2088 config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + '''
2089 #include <sys/mman.h>
2090 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }'''))
2091 config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + '''
2093 #if !defined(AT_EMPTY_PATH)
2094 # error missing definition
2096 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
2098 config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + '''
2099 #include <sys/mman.h>
2101 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }'''))
2103 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + '''
2104 #include <pthread.h>
2106 static void *f(void *p) { return NULL; }
2110 pthread_create(&thread, 0, f, 0);
2111 pthread_setname_np(thread, "QEMU");
2113 }''', dependencies: threads))
2114 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + '''
2115 #include <pthread.h>
2117 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
2121 pthread_create(&thread, 0, f, 0);
2123 }''', dependencies: threads))
2124 config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + '''
2125 #include <pthread.h>
2130 pthread_condattr_t attr
2131 pthread_condattr_init(&attr);
2132 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC);
2134 }''', dependencies: threads))
2135 config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + '''
2136 #include <pthread.h>
2138 static void *f(void *p) { return NULL; }
2141 int setsize = CPU_ALLOC_SIZE(64);
2144 pthread_create(&thread, 0, f, 0);
2145 cpuset = CPU_ALLOC(64);
2146 CPU_ZERO_S(setsize, cpuset);
2147 pthread_setaffinity_np(thread, setsize, cpuset);
2148 pthread_getaffinity_np(thread, setsize, cpuset);
2151 }''', dependencies: threads))
2152 config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + '''
2153 #include <sys/signalfd.h>
2155 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }'''))
2156 config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + '''
2164 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
2165 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
2169 config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + '''
2170 #include <sys/mman.h>
2172 return mlockall(MCL_FUTURE);
2176 if get_option('l2tpv3').allowed() and have_system
2177 have_l2tpv3 = cc.has_type('struct mmsghdr',
2178 prefix: gnu_source_prefix + '''
2179 #include <sys/socket.h>
2180 #include <linux/ip.h>''')
2182 config_host_data.set('CONFIG_L2TPV3', have_l2tpv3)
2185 if get_option('netmap').allowed() and have_system
2186 have_netmap = cc.compiles('''
2187 #include <inttypes.h>
2189 #include <net/netmap.h>
2190 #include <net/netmap_user.h>
2191 #if (NETMAP_API < 11) || (NETMAP_API > 15)
2194 int main(void) { return 0; }''')
2195 if not have_netmap and get_option('netmap').enabled()
2196 error('Netmap headers not available')
2199 config_host_data.set('CONFIG_NETMAP', have_netmap)
2201 # Work around a system header bug with some kernel/XFS header
2202 # versions where they both try to define 'struct fsxattr':
2203 # xfs headers will not try to redefine structs from linux headers
2204 # if this macro is set.
2205 config_host_data.set('HAVE_FSXATTR', cc.links('''
2206 #include <linux/fs.h>
2212 # Some versions of Mac OS X incorrectly define SIZE_MAX
2213 config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles('''
2217 return printf("%zu", SIZE_MAX);
2218 }''', args: ['-Werror']))
2225 y = __atomic_load_n(&x, __ATOMIC_RELAXED);
2226 __atomic_store_n(&x, y, __ATOMIC_RELAXED);
2227 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2228 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
2229 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
2233 # See if 64-bit atomic operations are supported.
2234 # Note that without __atomic builtins, we can only
2235 # assume atomic loads/stores max at pointer size.
2236 config_host_data.set('CONFIG_ATOMIC64', cc.links(atomic_test.format('uint64_t')))
2238 has_int128 = cc.links('''
2248 config_host_data.set('CONFIG_INT128', has_int128)
2251 # "do we have 128-bit atomics which are handled inline and specifically not
2252 # via libatomic". The reason we can't use libatomic is documented in the
2253 # comment starting "GCC is a house divided" in include/qemu/atomic128.h.
2254 has_atomic128 = cc.links(atomic_test.format('unsigned __int128'))
2256 config_host_data.set('CONFIG_ATOMIC128', has_atomic128)
2258 if not has_atomic128
2259 has_cmpxchg128 = cc.links('''
2262 unsigned __int128 x = 0, y = 0;
2263 __sync_val_compare_and_swap_16(&x, y, x);
2268 config_host_data.set('CONFIG_CMPXCHG128', has_cmpxchg128)
2272 config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + '''
2273 #include <sys/auxv.h>
2275 return getauxval(AT_HWCAP) == 0;
2278 config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles('''
2279 #include <linux/usbdevice_fs.h>
2281 #ifndef USBDEVFS_GET_CAPABILITIES
2282 #error "USBDEVFS_GET_CAPABILITIES undefined"
2285 #ifndef USBDEVFS_DISCONNECT_CLAIM
2286 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
2289 int main(void) { return 0; }'''))
2291 have_keyring = get_option('keyring') \
2292 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \
2293 .require(cc.compiles('''
2295 #include <asm/unistd.h>
2296 #include <linux/keyctl.h>
2297 #include <sys/syscall.h>
2300 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
2301 }'''), error_message: 'keyctl syscall not available on this system').allowed()
2302 config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring)
2304 have_cpuid_h = cc.links('''
2307 unsigned a, b, c, d;
2308 unsigned max = __get_cpuid_max(0, 0);
2311 __cpuid(1, a, b, c, d);
2315 __cpuid_count(7, 0, a, b, c, d);
2320 config_host_data.set('CONFIG_CPUID_H', have_cpuid_h)
2322 config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \
2323 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \
2324 .require(cc.links('''
2325 #pragma GCC push_options
2326 #pragma GCC target("avx2")
2328 #include <immintrin.h>
2329 static int bar(void *a) {
2330 __m256i x = *(__m256i *)a;
2331 return _mm256_testz_si256(x, x);
2333 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2334 '''), error_message: 'AVX2 not available').allowed())
2336 config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \
2337 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \
2338 .require(cc.links('''
2339 #pragma GCC push_options
2340 #pragma GCC target("avx512f")
2342 #include <immintrin.h>
2343 static int bar(void *a) {
2344 __m512i x = *(__m512i *)a;
2345 return _mm512_test_epi64_mask(x, x);
2347 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2348 '''), error_message: 'AVX512F not available').allowed())
2350 have_pvrdma = get_option('pvrdma') \
2351 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \
2352 .require(cc.compiles(gnu_source_prefix + '''
2353 #include <sys/mman.h>
2358 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
2361 }'''), error_message: 'PVRDMA requires mremap').allowed()
2364 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links('''
2365 #include <infiniband/verbs.h>
2369 struct ibv_pd *pd = NULL;
2375 mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
2381 if get_option('membarrier').disabled()
2382 have_membarrier = false
2383 elif targetos == 'windows'
2384 have_membarrier = true
2385 elif targetos == 'linux'
2386 have_membarrier = cc.compiles('''
2387 #include <linux/membarrier.h>
2388 #include <sys/syscall.h>
2392 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
2393 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
2397 config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \
2398 .require(have_membarrier, error_message: 'membarrier system call not available') \
2401 have_afalg = get_option('crypto_afalg') \
2402 .require(cc.compiles(gnu_source_prefix + '''
2404 #include <sys/types.h>
2405 #include <sys/socket.h>
2406 #include <linux/if_alg.h>
2409 sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
2412 '''), error_message: 'AF_ALG requested but could not be detected').allowed()
2413 config_host_data.set('CONFIG_AF_ALG', have_afalg)
2415 config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol(
2416 'linux/vm_sockets.h', 'AF_VSOCK',
2417 prefix: '#include <sys/socket.h>',
2421 have_vss_sdk = false # old xp/2003 SDK
2422 if targetos == 'windows' and link_language == 'cpp'
2423 have_vss = cxx.compiles('''
2424 #define __MIDL_user_allocate_free_DEFINED__
2426 int main(void) { return VSS_CTX_BACKUP; }''')
2427 have_vss_sdk = cxx.has_header('vscoordint.h')
2429 config_host_data.set('HAVE_VSS_SDK', have_vss_sdk)
2431 foreach k, v: config_host
2432 if k.startswith('CONFIG_')
2433 config_host_data.set(k, v == 'y' ? 1 : v)
2437 # Older versions of MinGW do not import _lock_file and _unlock_file properly.
2438 # This was fixed for v6.0.0 with commit b48e3ac8969d.
2439 if targetos == 'windows'
2440 config_host_data.set('HAVE__LOCK_FILE', cc.links('''
2446 }''', name: '_lock_file and _unlock_file'))
2449 ########################
2450 # Target configuration #
2451 ########################
2453 minikconf = find_program('scripts/minikconf.py')
2455 config_all_devices = {}
2456 config_all_disas = {}
2457 config_devices_mak_list = []
2458 config_devices_h = {}
2459 config_target_h = {}
2460 config_target_mak = {}
2463 'alpha' : ['CONFIG_ALPHA_DIS'],
2464 'avr' : ['CONFIG_AVR_DIS'],
2465 'cris' : ['CONFIG_CRIS_DIS'],
2466 'hexagon' : ['CONFIG_HEXAGON_DIS'],
2467 'hppa' : ['CONFIG_HPPA_DIS'],
2468 'i386' : ['CONFIG_I386_DIS'],
2469 'x86_64' : ['CONFIG_I386_DIS'],
2470 'm68k' : ['CONFIG_M68K_DIS'],
2471 'microblaze' : ['CONFIG_MICROBLAZE_DIS'],
2472 'mips' : ['CONFIG_MIPS_DIS'],
2473 'nios2' : ['CONFIG_NIOS2_DIS'],
2474 'or1k' : ['CONFIG_OPENRISC_DIS'],
2475 'ppc' : ['CONFIG_PPC_DIS'],
2476 'riscv' : ['CONFIG_RISCV_DIS'],
2477 'rx' : ['CONFIG_RX_DIS'],
2478 's390' : ['CONFIG_S390_DIS'],
2479 'sh4' : ['CONFIG_SH4_DIS'],
2480 'sparc' : ['CONFIG_SPARC_DIS'],
2481 'xtensa' : ['CONFIG_XTENSA_DIS'],
2482 'loongarch' : ['CONFIG_LOONGARCH_DIS'],
2484 if link_language == 'cpp'
2486 'mips' : [ 'CONFIG_MIPS_DIS', 'CONFIG_NANOMIPS_DIS'],
2490 have_ivshmem = config_host_data.get('CONFIG_EVENTFD')
2492 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \
2493 (have_tpm ? ['CONFIG_TPM=y'] : []) + \
2494 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \
2495 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \
2496 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \
2497 (x11.found() ? ['CONFIG_X11=y'] : []) + \
2498 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \
2499 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \
2500 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \
2501 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \
2502 ('CONFIG_LINUX' in config_host ? ['CONFIG_LINUX=y'] : []) + \
2503 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \
2504 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \
2505 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : [])
2507 ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ]
2509 default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host
2510 actual_target_dirs = []
2512 foreach target : target_dirs
2513 config_target = { 'TARGET_NAME': target.split('-')[0] }
2514 if target.endswith('linux-user')
2515 if targetos != 'linux'
2519 error('Target @0@ is only available on a Linux host'.format(target))
2521 config_target += { 'CONFIG_LINUX_USER': 'y' }
2522 elif target.endswith('bsd-user')
2523 if 'CONFIG_BSD' not in config_host
2527 error('Target @0@ is only available on a BSD host'.format(target))
2529 config_target += { 'CONFIG_BSD_USER': 'y' }
2530 elif target.endswith('softmmu')
2531 config_target += { 'CONFIG_SOFTMMU': 'y' }
2533 if target.endswith('-user')
2535 'CONFIG_USER_ONLY': 'y',
2536 'CONFIG_QEMU_INTERP_PREFIX':
2537 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME'])
2542 foreach sym: accelerators
2543 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, [])
2544 config_target += { sym: 'y' }
2545 config_all += { sym: 'y' }
2546 if sym == 'CONFIG_TCG' and tcg_arch == 'tci'
2547 config_target += { 'CONFIG_TCG_INTERPRETER': 'y' }
2549 if target in modular_tcg
2550 config_target += { 'CONFIG_TCG_MODULAR': 'y' }
2552 config_target += { 'CONFIG_TCG_BUILTIN': 'y' }
2554 accel_kconfig += [ sym + '=y' ]
2557 if accel_kconfig.length() == 0
2561 error('No accelerator available for target @0@'.format(target))
2564 actual_target_dirs += target
2565 config_target += keyval.load('configs/targets' / target + '.mak')
2566 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' }
2568 if 'TARGET_NEED_FDT' in config_target
2569 fdt_required += target
2573 if 'TARGET_BASE_ARCH' not in config_target
2574 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']}
2576 if 'TARGET_ABI_DIR' not in config_target
2577 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']}
2579 if 'TARGET_BIG_ENDIAN' not in config_target
2580 config_target += {'TARGET_BIG_ENDIAN': 'n'}
2583 foreach k, v: disassemblers
2584 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k)
2586 config_target += { sym: 'y' }
2587 config_all_disas += { sym: 'y' }
2592 config_target_data = configuration_data()
2593 foreach k, v: config_target
2594 if not k.startswith('TARGET_') and not k.startswith('CONFIG_')
2596 elif ignored.contains(k)
2598 elif k == 'TARGET_BASE_ARCH'
2599 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is
2600 # not used to select files from sourcesets.
2601 config_target_data.set('TARGET_' + v.to_upper(), 1)
2602 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX'
2603 config_target_data.set_quoted(k, v)
2605 config_target_data.set(k, 1)
2607 config_target_data.set(k, 0)
2609 config_target_data.set(k, v)
2612 config_target_data.set('QEMU_ARCH',
2613 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper())
2614 config_target_h += {target: configure_file(output: target + '-config-target.h',
2615 configuration: config_target_data)}
2617 if target.endswith('-softmmu')
2618 config_input = meson.get_external_property(target, 'default')
2619 config_devices_mak = target + '-config-devices.mak'
2620 config_devices_mak = configure_file(
2621 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'],
2622 output: config_devices_mak,
2623 depfile: config_devices_mak + '.d',
2625 command: [minikconf,
2626 get_option('default_devices') ? '--defconfig' : '--allnoconfig',
2627 config_devices_mak, '@DEPFILE@', '@INPUT@',
2628 host_kconfig, accel_kconfig,
2629 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y'])
2631 config_devices_data = configuration_data()
2632 config_devices = keyval.load(config_devices_mak)
2633 foreach k, v: config_devices
2634 config_devices_data.set(k, 1)
2636 config_devices_mak_list += config_devices_mak
2637 config_devices_h += {target: configure_file(output: target + '-config-devices.h',
2638 configuration: config_devices_data)}
2639 config_target += config_devices
2640 config_all_devices += config_devices
2642 config_target_mak += {target: config_target}
2644 target_dirs = actual_target_dirs
2646 # This configuration is used to build files that are shared by
2647 # multiple binaries, and then extracted out of the "common"
2648 # static_library target.
2650 # We do not use all_sources()/all_dependencies(), because it would
2651 # build literally all source files, including devices only used by
2652 # targets that are not built for this compilation. The CONFIG_ALL
2653 # pseudo symbol replaces it.
2655 config_all += config_all_devices
2656 config_all += config_host
2657 config_all += config_all_disas
2659 'CONFIG_XEN': xen.found(),
2660 'CONFIG_SOFTMMU': have_system,
2661 'CONFIG_USER_ONLY': have_user,
2665 target_configs_h = []
2666 foreach target: target_dirs
2667 target_configs_h += config_target_h[target]
2668 target_configs_h += config_devices_h.get(target, [])
2670 genh += custom_target('config-poison.h',
2671 input: [target_configs_h],
2672 output: 'config-poison.h',
2674 command: [find_program('scripts/make-config-poison.sh'),
2681 capstone = not_found
2682 if not get_option('capstone').auto() or have_system or have_user
2683 capstone = dependency('capstone', version: '>=3.0.5',
2684 kwargs: static_kwargs, method: 'pkg-config',
2685 required: get_option('capstone'))
2687 # Some versions of capstone have broken pkg-config file
2688 # that reports a wrong -I path, causing the #include to
2689 # fail later. If the system has such a broken version
2691 if capstone.found() and not cc.compiles('#include <capstone.h>',
2692 dependencies: [capstone])
2693 capstone = not_found
2694 if get_option('capstone').enabled()
2695 error('capstone requested, but it does not appear to work')
2700 libvfio_user_dep = not_found
2701 if have_system and vfio_user_server_allowed
2702 have_internal = fs.exists(meson.current_source_dir() / 'subprojects/libvfio-user/meson.build')
2704 if not have_internal
2705 error('libvfio-user source not found - please pull git submodule')
2708 libvfio_user_proj = subproject('libvfio-user')
2710 libvfio_user_lib = libvfio_user_proj.get_variable('libvfio_user_dep')
2712 libvfio_user_dep = declare_dependency(dependencies: [libvfio_user_lib])
2717 fdt_opt = get_option('fdt')
2718 if fdt_opt in ['enabled', 'auto', 'system']
2719 have_internal = fs.exists(meson.current_source_dir() / 'dtc/libfdt/Makefile.libfdt')
2720 fdt = cc.find_library('fdt', kwargs: static_kwargs,
2721 required: fdt_opt == 'system' or
2722 fdt_opt == 'enabled' and not have_internal)
2723 if fdt.found() and cc.links('''
2725 #include <libfdt_env.h>
2726 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''',
2729 elif fdt_opt == 'system'
2730 error('system libfdt requested, but it is too old (1.5.1 or newer required)')
2732 fdt_opt = 'internal'
2734 fdt_opt = 'disabled'
2738 if fdt_opt == 'internal'
2741 'dtc/libfdt/fdt_ro.c',
2742 'dtc/libfdt/fdt_wip.c',
2743 'dtc/libfdt/fdt_sw.c',
2744 'dtc/libfdt/fdt_rw.c',
2745 'dtc/libfdt/fdt_strerror.c',
2746 'dtc/libfdt/fdt_empty_tree.c',
2747 'dtc/libfdt/fdt_addresses.c',
2748 'dtc/libfdt/fdt_overlay.c',
2749 'dtc/libfdt/fdt_check.c',
2752 fdt_inc = include_directories('dtc/libfdt')
2753 libfdt = static_library('fdt',
2754 build_by_default: false,
2756 include_directories: fdt_inc)
2757 fdt = declare_dependency(link_with: libfdt,
2758 include_directories: fdt_inc)
2761 fdt_opt = 'disabled'
2763 if not fdt.found() and fdt_required.length() > 0
2764 error('fdt not available but required by targets ' + ', '.join(fdt_required))
2767 config_host_data.set('CONFIG_CAPSTONE', capstone.found())
2768 config_host_data.set('CONFIG_FDT', fdt.found())
2769 config_host_data.set('CONFIG_SLIRP', slirp.found())
2771 #####################
2772 # Generated sources #
2773 #####################
2775 genh += configure_file(output: 'config-host.h', configuration: config_host_data)
2777 hxtool = find_program('scripts/hxtool')
2778 shaderinclude = find_program('scripts/shaderinclude.py')
2779 qapi_gen = find_program('scripts/qapi-gen.py')
2780 qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py',
2781 meson.current_source_dir() / 'scripts/qapi/commands.py',
2782 meson.current_source_dir() / 'scripts/qapi/common.py',
2783 meson.current_source_dir() / 'scripts/qapi/error.py',
2784 meson.current_source_dir() / 'scripts/qapi/events.py',
2785 meson.current_source_dir() / 'scripts/qapi/expr.py',
2786 meson.current_source_dir() / 'scripts/qapi/gen.py',
2787 meson.current_source_dir() / 'scripts/qapi/introspect.py',
2788 meson.current_source_dir() / 'scripts/qapi/parser.py',
2789 meson.current_source_dir() / 'scripts/qapi/schema.py',
2790 meson.current_source_dir() / 'scripts/qapi/source.py',
2791 meson.current_source_dir() / 'scripts/qapi/types.py',
2792 meson.current_source_dir() / 'scripts/qapi/visit.py',
2793 meson.current_source_dir() / 'scripts/qapi/common.py',
2794 meson.current_source_dir() / 'scripts/qapi-gen.py'
2798 python, files('scripts/tracetool.py'),
2799 '--backend=' + ','.join(get_option('trace_backends'))
2801 tracetool_depends = files(
2802 'scripts/tracetool/backend/log.py',
2803 'scripts/tracetool/backend/__init__.py',
2804 'scripts/tracetool/backend/dtrace.py',
2805 'scripts/tracetool/backend/ftrace.py',
2806 'scripts/tracetool/backend/simple.py',
2807 'scripts/tracetool/backend/syslog.py',
2808 'scripts/tracetool/backend/ust.py',
2809 'scripts/tracetool/format/ust_events_c.py',
2810 'scripts/tracetool/format/ust_events_h.py',
2811 'scripts/tracetool/format/__init__.py',
2812 'scripts/tracetool/format/d.py',
2813 'scripts/tracetool/format/simpletrace_stap.py',
2814 'scripts/tracetool/format/c.py',
2815 'scripts/tracetool/format/h.py',
2816 'scripts/tracetool/format/log_stap.py',
2817 'scripts/tracetool/format/stap.py',
2818 'scripts/tracetool/__init__.py',
2819 'scripts/tracetool/transform.py',
2820 'scripts/tracetool/vcpu.py'
2823 qemu_version_cmd = [find_program('scripts/qemu-version.sh'),
2824 meson.current_source_dir(),
2825 get_option('pkgversion'), meson.project_version()]
2826 qemu_version = custom_target('qemu-version.h',
2827 output: 'qemu-version.h',
2828 command: qemu_version_cmd,
2830 build_by_default: true,
2831 build_always_stale: true)
2832 genh += qemu_version
2836 ['qemu-options.hx', 'qemu-options.def'],
2837 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'],
2841 ['hmp-commands.hx', 'hmp-commands.h'],
2842 ['hmp-commands-info.hx', 'hmp-commands-info.h'],
2845 foreach d : hx_headers
2846 hxdep += custom_target(d[1],
2850 build_by_default: true, # to be removed when added to a target
2851 command: [hxtool, '-h', '@INPUT0@'])
2859 authz_ss = ss.source_set()
2860 blockdev_ss = ss.source_set()
2861 block_ss = ss.source_set()
2862 chardev_ss = ss.source_set()
2863 common_ss = ss.source_set()
2864 crypto_ss = ss.source_set()
2865 hwcore_ss = ss.source_set()
2866 io_ss = ss.source_set()
2867 qmp_ss = ss.source_set()
2868 qom_ss = ss.source_set()
2869 softmmu_ss = ss.source_set()
2870 specific_fuzz_ss = ss.source_set()
2871 specific_ss = ss.source_set()
2872 stub_ss = ss.source_set()
2873 trace_ss = ss.source_set()
2874 user_ss = ss.source_set()
2875 util_ss = ss.source_set()
2878 qtest_module_ss = ss.source_set()
2879 tcg_module_ss = ss.source_set()
2885 target_softmmu_arch = {}
2886 target_user_arch = {}
2892 # TODO: add each directory to the subdirs from its own meson.build, once
2894 trace_events_subdirs = [
2903 trace_events_subdirs += [ 'linux-user' ]
2906 trace_events_subdirs += [ 'bsd-user' ]
2909 trace_events_subdirs += [
2918 trace_events_subdirs += [
2932 'hw/block/dataplane',
2981 if have_system or have_user
2982 trace_events_subdirs += [
3000 vhost_user = not_found
3001 if targetos == 'linux' and have_vhost_user
3002 libvhost_user = subproject('libvhost-user')
3003 vhost_user = libvhost_user.get_variable('vhost_user_dep')
3006 libvduse = not_found
3008 libvduse_proj = subproject('libvduse')
3009 libvduse = libvduse_proj.get_variable('libvduse_dep')
3012 # NOTE: the trace/ subdirectory needs the qapi_trace_events variable
3013 # that is filled in by qapi/.
3028 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO')
3029 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO')
3032 qom_ss = qom_ss.apply(config_host, strict: false)
3033 libqom = static_library('qom', qom_ss.sources() + genh,
3034 dependencies: [qom_ss.dependencies()],
3036 qom = declare_dependency(link_whole: libqom)
3038 event_loop_base = files('event-loop-base.c')
3039 event_loop_base = static_library('event-loop-base', sources: event_loop_base + genh,
3040 build_by_default: true)
3041 event_loop_base = declare_dependency(link_whole: event_loop_base,
3042 dependencies: [qom])
3044 stub_ss = stub_ss.apply(config_all, strict: false)
3046 util_ss.add_all(trace_ss)
3047 util_ss = util_ss.apply(config_all, strict: false)
3048 libqemuutil = static_library('qemuutil',
3049 sources: util_ss.sources() + stub_ss.sources() + genh,
3050 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman])
3051 qemuutil = declare_dependency(link_with: libqemuutil,
3052 sources: genh + version_res,
3053 dependencies: [event_loop_base])
3055 if have_system or have_user
3056 decodetree = generator(find_program('scripts/decodetree.py'),
3057 output: 'decode-@BASENAME@.c.inc',
3058 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@'])
3059 subdir('libdecnumber')
3076 if config_host_data.get('CONFIG_REPLICATION')
3077 block_ss.add(files('replication.c'))
3084 blockdev_ss.add(files(
3091 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon,
3092 # os-win32.c does not
3093 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c'))
3094 softmmu_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')])
3097 common_ss.add(files('cpus-common.c'))
3101 common_ss.add(capstone)
3102 specific_ss.add(files('cpu.c', 'disas.c'), capstone)
3104 # Work around a gcc bug/misfeature wherein constant propagation looks
3106 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696
3107 # to guess that a const variable is always zero. Without lto, this is
3108 # impossible, as the alias is restricted to page-vary-common.c. Indeed,
3109 # without lto, not even the alias is required -- we simply use different
3110 # declarations in different compilation units.
3111 pagevary = files('page-vary-common.c')
3112 if get_option('b_lto')
3113 pagevary_flags = ['-fno-lto']
3114 if get_option('cfi')
3115 pagevary_flags += '-fno-sanitize=cfi-icall'
3117 pagevary = static_library('page-vary-common', sources: pagevary + genh,
3118 c_args: pagevary_flags)
3119 pagevary = declare_dependency(link_with: pagevary)
3121 common_ss.add(pagevary)
3122 specific_ss.add(files('page-vary.c'))
3130 subdir('semihosting')
3137 common_user_inc = []
3139 subdir('common-user')
3141 subdir('linux-user')
3143 # needed for fuzzing binaries
3144 subdir('tests/qtest/libqos')
3145 subdir('tests/qtest/fuzz')
3148 tcg_real_module_ss = ss.source_set()
3149 tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss)
3150 specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss)
3151 target_modules += { 'accel' : { 'qtest': qtest_module_ss,
3152 'tcg': tcg_real_module_ss }}
3154 ########################
3155 # Library dependencies #
3156 ########################
3158 modinfo_collect = find_program('scripts/modinfo-collect.py')
3159 modinfo_generate = find_program('scripts/modinfo-generate.py')
3164 foreach d, list : modules
3165 if not (d == 'block' ? have_block : have_system)
3169 foreach m, module_ss : list
3170 if enable_modules and targetos != 'windows'
3171 module_ss = module_ss.apply(config_all, strict: false)
3172 sl = static_library(d + '-' + m, [genh, module_ss.sources()],
3173 dependencies: [modulecommon, module_ss.dependencies()], pic: true)
3179 if module_ss.sources() != []
3180 # FIXME: Should use sl.extract_all_objects(recursive: true) as
3181 # input. Sources can be used multiple times but objects are
3182 # unique when it comes to lookup in compile_commands.json.
3183 # Depnds on a mesion version with
3184 # https://github.com/mesonbuild/meson/pull/8900
3185 modinfo_files += custom_target(d + '-' + m + '.modinfo',
3186 output: d + '-' + m + '.modinfo',
3187 input: module_ss.sources() + genh,
3189 command: [modinfo_collect, module_ss.sources()])
3193 block_ss.add_all(module_ss)
3195 softmmu_ss.add_all(module_ss)
3201 foreach d, list : target_modules
3202 foreach m, module_ss : list
3203 if enable_modules and targetos != 'windows'
3204 foreach target : target_dirs
3205 if target.endswith('-softmmu')
3206 config_target = config_target_mak[target]
3207 config_target += config_host
3208 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3209 c_args = ['-DNEED_CPU_H',
3210 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3211 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3212 target_module_ss = module_ss.apply(config_target, strict: false)
3213 if target_module_ss.sources() != []
3214 module_name = d + '-' + m + '-' + config_target['TARGET_NAME']
3215 sl = static_library(module_name,
3216 [genh, target_module_ss.sources()],
3217 dependencies: [modulecommon, target_module_ss.dependencies()],
3218 include_directories: target_inc,
3222 # FIXME: Should use sl.extract_all_objects(recursive: true) too.
3223 modinfo_files += custom_target(module_name + '.modinfo',
3224 output: module_name + '.modinfo',
3225 input: target_module_ss.sources() + genh,
3227 command: [modinfo_collect, '--target', target, target_module_ss.sources()])
3232 specific_ss.add_all(module_ss)
3238 foreach target : target_dirs
3239 if target.endswith('-softmmu')
3240 config_target = config_target_mak[target]
3241 config_devices_mak = target + '-config-devices.mak'
3242 modinfo_src = custom_target('modinfo-' + target + '.c',
3243 output: 'modinfo-' + target + '.c',
3244 input: modinfo_files,
3245 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'],
3248 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src)
3249 modinfo_dep = declare_dependency(link_with: modinfo_lib)
3251 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH']
3252 hw_arch[arch].add(modinfo_dep)
3257 nm = find_program('nm')
3258 undefsym = find_program('scripts/undefsym.py')
3259 block_syms = custom_target('block.syms', output: 'block.syms',
3260 input: [libqemuutil, block_mods],
3262 command: [undefsym, nm, '@INPUT@'])
3263 qemu_syms = custom_target('qemu.syms', output: 'qemu.syms',
3264 input: [libqemuutil, softmmu_mods],
3266 command: [undefsym, nm, '@INPUT@'])
3268 authz_ss = authz_ss.apply(config_host, strict: false)
3269 libauthz = static_library('authz', authz_ss.sources() + genh,
3270 dependencies: [authz_ss.dependencies()],
3272 build_by_default: false)
3274 authz = declare_dependency(link_whole: libauthz,
3277 crypto_ss = crypto_ss.apply(config_host, strict: false)
3278 libcrypto = static_library('crypto', crypto_ss.sources() + genh,
3279 dependencies: [crypto_ss.dependencies()],
3281 build_by_default: false)
3283 crypto = declare_dependency(link_whole: libcrypto,
3284 dependencies: [authz, qom])
3286 io_ss = io_ss.apply(config_host, strict: false)
3287 libio = static_library('io', io_ss.sources() + genh,
3288 dependencies: [io_ss.dependencies()],
3289 link_with: libqemuutil,
3291 build_by_default: false)
3293 io = declare_dependency(link_whole: libio, dependencies: [crypto, qom])
3295 libmigration = static_library('migration', sources: migration_files + genh,
3297 build_by_default: false)
3298 migration = declare_dependency(link_with: libmigration,
3299 dependencies: [zlib, qom, io])
3300 softmmu_ss.add(migration)
3302 block_ss = block_ss.apply(config_host, strict: false)
3303 libblock = static_library('block', block_ss.sources() + genh,
3304 dependencies: block_ss.dependencies(),
3305 link_depends: block_syms,
3307 build_by_default: false)
3309 block = declare_dependency(link_whole: [libblock],
3310 link_args: '@block.syms',
3311 dependencies: [crypto, io])
3313 blockdev_ss = blockdev_ss.apply(config_host, strict: false)
3314 libblockdev = static_library('blockdev', blockdev_ss.sources() + genh,
3315 dependencies: blockdev_ss.dependencies(),
3317 build_by_default: false)
3319 blockdev = declare_dependency(link_whole: [libblockdev],
3320 dependencies: [block, event_loop_base])
3322 qmp_ss = qmp_ss.apply(config_host, strict: false)
3323 libqmp = static_library('qmp', qmp_ss.sources() + genh,
3324 dependencies: qmp_ss.dependencies(),
3326 build_by_default: false)
3328 qmp = declare_dependency(link_whole: [libqmp])
3330 libchardev = static_library('chardev', chardev_ss.sources() + genh,
3332 dependencies: chardev_ss.dependencies(),
3333 build_by_default: false)
3335 chardev = declare_dependency(link_whole: libchardev)
3337 hwcore_ss = hwcore_ss.apply(config_host, strict: false)
3338 libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh,
3340 build_by_default: false)
3341 hwcore = declare_dependency(link_whole: libhwcore)
3342 common_ss.add(hwcore)
3348 emulator_modules = []
3349 foreach m : block_mods + softmmu_mods
3350 emulator_modules += shared_module(m.name(),
3351 build_by_default: true,
3355 install_dir: qemu_moddir)
3357 if emulator_modules.length() > 0
3358 alias_target('modules', emulator_modules)
3361 softmmu_ss.add(authz, blockdev, chardev, crypto, io, qmp)
3362 common_ss.add(qom, qemuutil)
3364 common_ss.add_all(when: 'CONFIG_SOFTMMU', if_true: [softmmu_ss])
3365 common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss)
3367 common_all = common_ss.apply(config_all, strict: false)
3368 common_all = static_library('common',
3369 build_by_default: false,
3370 sources: common_all.sources() + genh,
3371 include_directories: common_user_inc,
3372 implicit_include_directories: false,
3373 dependencies: common_all.dependencies(),
3376 feature_to_c = find_program('scripts/feature_to_c.sh')
3378 if targetos == 'darwin'
3379 entitlement = find_program('scripts/entitlement.sh')
3383 foreach target : target_dirs
3384 config_target = config_target_mak[target]
3385 target_name = config_target['TARGET_NAME']
3386 target_base_arch = config_target['TARGET_BASE_ARCH']
3387 arch_srcs = [config_target_h[target]]
3389 c_args = ['-DNEED_CPU_H',
3390 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3391 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3392 link_args = emulator_link_args
3394 config_target += config_host
3395 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3396 if targetos == 'linux'
3397 target_inc += include_directories('linux-headers', is_system: true)
3399 if target.endswith('-softmmu')
3400 target_type='system'
3401 t = target_softmmu_arch[target_base_arch].apply(config_target, strict: false)
3402 arch_srcs += t.sources()
3403 arch_deps += t.dependencies()
3405 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch
3406 hw = hw_arch[hw_dir].apply(config_target, strict: false)
3407 arch_srcs += hw.sources()
3408 arch_deps += hw.dependencies()
3410 arch_srcs += config_devices_h[target]
3411 link_args += ['@block.syms', '@qemu.syms']
3413 abi = config_target['TARGET_ABI_DIR']
3415 target_inc += common_user_inc
3416 if target_base_arch in target_user_arch
3417 t = target_user_arch[target_base_arch].apply(config_target, strict: false)
3418 arch_srcs += t.sources()
3419 arch_deps += t.dependencies()
3421 if 'CONFIG_LINUX_USER' in config_target
3422 base_dir = 'linux-user'
3424 if 'CONFIG_BSD_USER' in config_target
3425 base_dir = 'bsd-user'
3426 target_inc += include_directories('bsd-user/' / targetos)
3427 target_inc += include_directories('bsd-user/host/' / host_arch)
3428 dir = base_dir / abi
3429 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c')
3431 target_inc += include_directories(
3435 if 'CONFIG_LINUX_USER' in config_target
3436 dir = base_dir / abi
3437 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c')
3438 if config_target.has_key('TARGET_SYSTBL_ABI')
3440 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'],
3441 extra_args : config_target['TARGET_SYSTBL_ABI'])
3446 if 'TARGET_XML_FILES' in config_target
3447 gdbstub_xml = custom_target(target + '-gdbstub-xml.c',
3448 output: target + '-gdbstub-xml.c',
3449 input: files(config_target['TARGET_XML_FILES'].split()),
3450 command: [feature_to_c, '@INPUT@'],
3452 arch_srcs += gdbstub_xml
3455 t = target_arch[target_base_arch].apply(config_target, strict: false)
3456 arch_srcs += t.sources()
3457 arch_deps += t.dependencies()
3459 target_common = common_ss.apply(config_target, strict: false)
3460 objects = common_all.extract_objects(target_common.sources())
3461 deps = target_common.dependencies()
3463 target_specific = specific_ss.apply(config_target, strict: false)
3464 arch_srcs += target_specific.sources()
3465 arch_deps += target_specific.dependencies()
3467 lib = static_library('qemu-' + target,
3468 sources: arch_srcs + genh,
3469 dependencies: arch_deps,
3471 include_directories: target_inc,
3473 build_by_default: false,
3476 if target.endswith('-softmmu')
3478 'name': 'qemu-system-' + target_name,
3479 'win_subsystem': 'console',
3480 'sources': files('softmmu/main.c'),
3483 if targetos == 'windows' and (sdl.found() or gtk.found())
3485 'name': 'qemu-system-' + target_name + 'w',
3486 'win_subsystem': 'windows',
3487 'sources': files('softmmu/main.c'),
3491 if get_option('fuzzing')
3492 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false)
3494 'name': 'qemu-fuzz-' + target_name,
3495 'win_subsystem': 'console',
3496 'sources': specific_fuzz.sources(),
3497 'dependencies': specific_fuzz.dependencies(),
3502 'name': 'qemu-' + target_name,
3503 'win_subsystem': 'console',
3509 exe_name = exe['name']
3510 if targetos == 'darwin'
3511 exe_name += '-unsigned'
3514 emulator = executable(exe_name, exe['sources'],
3517 dependencies: arch_deps + deps + exe['dependencies'],
3518 objects: lib.extract_all_objects(recursive: true),
3519 link_language: link_language,
3520 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []),
3521 link_args: link_args,
3522 win_subsystem: exe['win_subsystem'])
3524 if targetos == 'darwin'
3525 icon = 'pc-bios/qemu.rsrc'
3526 build_input = [emulator, files(icon)]
3528 get_option('bindir') / exe_name,
3529 meson.current_source_dir() / icon
3531 if 'CONFIG_HVF' in config_target
3532 entitlements = 'accel/hvf/entitlements.plist'
3533 build_input += files(entitlements)
3534 install_input += meson.current_source_dir() / entitlements
3537 emulators += {exe['name'] : custom_target(exe['name'],
3539 output: exe['name'],
3540 command: [entitlement, '@OUTPUT@', '@INPUT@'])
3543 meson.add_install_script(entitlement, '--install',
3544 get_option('bindir') / exe['name'],
3547 emulators += {exe['name']: emulator}
3552 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false},
3553 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true},
3554 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true},
3555 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true},
3557 custom_target(exe['name'] + stp['ext'],
3558 input: trace_events_all,
3559 output: exe['name'] + stp['ext'],
3560 install: stp['install'],
3561 install_dir: get_option('datadir') / 'systemtap/tapset',
3563 tracetool, '--group=all', '--format=' + stp['fmt'],
3564 '--binary=' + stp['bin'],
3565 '--target-name=' + target_name,
3566 '--target-type=' + target_type,
3567 '--probe-prefix=qemu.' + target_type + '.' + target_name,
3568 '@INPUT@', '@OUTPUT@'
3570 depend_files: tracetool_depends)
3576 # Other build targets
3578 if 'CONFIG_PLUGIN' in config_host
3579 install_headers('include/qemu/qemu-plugin.h')
3584 # Don't build qemu-keymap if xkbcommon is not explicitly enabled
3585 # when we don't build tools or system
3586 if xkbcommon.found()
3587 # used for the update-keymaps target, so include rules even if !have_tools
3588 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh,
3589 dependencies: [qemuutil, xkbcommon], install: have_tools)
3593 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep],
3594 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true)
3595 qemu_io = executable('qemu-io', files('qemu-io.c'),
3596 dependencies: [block, qemuutil], install: true)
3597 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'),
3598 dependencies: [blockdev, qemuutil, gnutls, selinux],
3601 subdir('storage-daemon')
3602 subdir('contrib/rdmacm-mux')
3603 subdir('contrib/elf2dmp')
3605 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'),
3606 dependencies: qemuutil,
3610 subdir('contrib/vhost-user-blk')
3611 subdir('contrib/vhost-user-gpu')
3612 subdir('contrib/vhost-user-input')
3613 subdir('contrib/vhost-user-scsi')
3616 if targetos == 'linux'
3617 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'),
3618 dependencies: [qemuutil, libcap_ng],
3620 install_dir: get_option('libexecdir'))
3622 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'),
3623 dependencies: [authz, crypto, io, qom, qemuutil,
3624 libcap_ng, mpathpersist],
3629 subdir('contrib/ivshmem-client')
3630 subdir('contrib/ivshmem-server')
3643 if host_machine.system() == 'windows'
3645 find_program('scripts/nsis.py'),
3647 get_option('prefix'),
3648 meson.current_source_dir(),
3649 config_host['GLIB_BINDIR'],
3652 '-DDISPLAYVERSION=' + meson.project_version(),
3655 nsis_cmd += '-DCONFIG_DOCUMENTATION=y'
3658 nsis_cmd += '-DCONFIG_GTK=y'
3661 nsis = custom_target('nsis',
3662 output: 'qemu-setup-' + meson.project_version() + '.exe',
3663 input: files('qemu.nsi'),
3664 build_always_stale: true,
3665 command: nsis_cmd + ['@INPUT@'])
3666 alias_target('installer', nsis)
3669 #########################
3670 # Configuration summary #
3671 #########################
3675 summary_info += {'Install prefix': get_option('prefix')}
3676 summary_info += {'BIOS directory': qemu_datadir}
3677 pathsep = targetos == 'windows' ? ';' : ':'
3678 summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))}
3679 summary_info += {'binary directory': get_option('prefix') / get_option('bindir')}
3680 summary_info += {'library directory': get_option('prefix') / get_option('libdir')}
3681 summary_info += {'module directory': qemu_moddir}
3682 summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')}
3683 summary_info += {'include directory': get_option('prefix') / get_option('includedir')}
3684 summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')}
3685 if targetos != 'windows'
3686 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')}
3687 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')}
3689 summary_info += {'local state directory': 'queried at runtime'}
3691 summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')}
3692 summary_info += {'Build directory': meson.current_build_dir()}
3693 summary_info += {'Source path': meson.current_source_dir()}
3694 summary_info += {'GIT submodules': config_host['GIT_SUBMODULES']}
3695 summary(summary_info, bool_yn: true, section: 'Directories')
3699 summary_info += {'git': config_host['GIT']}
3700 summary_info += {'make': config_host['MAKE']}
3701 summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())}
3702 summary_info += {'sphinx-build': sphinx_build}
3703 if config_host.has_key('HAVE_GDB_BIN')
3704 summary_info += {'gdb': config_host['HAVE_GDB_BIN']}
3706 summary_info += {'iasl': iasl}
3707 summary_info += {'genisoimage': config_host['GENISOIMAGE']}
3708 if targetos == 'windows' and have_ga
3709 summary_info += {'wixl': wixl}
3711 if slirp.found() and have_system
3712 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false}
3714 summary(summary_info, bool_yn: true, section: 'Host binaries')
3716 # Configurable features
3718 summary_info += {'Documentation': build_docs}
3719 summary_info += {'system-mode emulation': have_system}
3720 summary_info += {'user-mode emulation': have_user}
3721 summary_info += {'block layer': have_block}
3722 summary_info += {'Install blobs': get_option('install_blobs')}
3723 summary_info += {'module support': config_host.has_key('CONFIG_MODULES')}
3724 if config_host.has_key('CONFIG_MODULES')
3725 summary_info += {'alternative module path': get_option('module_upgrades')}
3727 summary_info += {'fuzzing support': get_option('fuzzing')}
3729 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)}
3731 summary_info += {'Trace backends': ','.join(get_option('trace_backends'))}
3732 if 'simple' in get_option('trace_backends')
3733 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'}
3735 summary_info += {'D-Bus display': dbus_display}
3736 summary_info += {'QOM debugging': get_option('qom_cast_debug')}
3737 summary_info += {'vhost-kernel support': have_vhost_kernel}
3738 summary_info += {'vhost-net support': have_vhost_net}
3739 summary_info += {'vhost-user support': have_vhost_user}
3740 summary_info += {'vhost-user-crypto support': have_vhost_user_crypto}
3741 summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server}
3742 summary_info += {'vhost-vdpa support': have_vhost_vdpa}
3743 summary_info += {'build guest agent': have_ga}
3744 summary(summary_info, bool_yn: true, section: 'Configurable features')
3746 # Compilation information
3748 summary_info += {'host CPU': cpu}
3749 summary_info += {'host endianness': build_machine.endian()}
3750 summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())}
3751 summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())}
3752 if link_language == 'cpp'
3753 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())}
3755 summary_info += {'C++ compiler': false}
3757 if targetos == 'darwin'
3758 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())}
3760 summary_info += {'CFLAGS': ' '.join(get_option('c_args')
3761 + ['-O' + get_option('optimization')]
3762 + (get_option('debug') ? ['-g'] : []))}
3763 if link_language == 'cpp'
3764 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args')
3765 + ['-O' + get_option('optimization')]
3766 + (get_option('debug') ? ['-g'] : []))}
3768 if targetos == 'darwin'
3769 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args')
3770 + ['-O' + get_option('optimization')]
3771 + (get_option('debug') ? ['-g'] : []))}
3773 link_args = get_option(link_language + '_link_args')
3774 if link_args.length() > 0
3775 summary_info += {'LDFLAGS': ' '.join(link_args)}
3777 summary_info += {'QEMU_CFLAGS': ' '.join(qemu_cflags)}
3778 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_cxxflags)}
3779 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_objcflags)}
3780 summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)}
3781 summary_info += {'profiler': get_option('profiler')}
3782 summary_info += {'link-time optimization (LTO)': get_option('b_lto')}
3783 summary_info += {'PIE': get_option('b_pie')}
3784 summary_info += {'static build': config_host.has_key('CONFIG_STATIC')}
3785 summary_info += {'malloc trim support': has_malloc_trim}
3786 summary_info += {'membarrier': have_membarrier}
3787 summary_info += {'debug stack usage': get_option('debug_stack_usage')}
3788 summary_info += {'mutex debugging': get_option('debug_mutex')}
3789 summary_info += {'memory allocator': get_option('malloc')}
3790 summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')}
3791 summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')}
3792 summary_info += {'gprof enabled': get_option('gprof')}
3793 summary_info += {'gcov': get_option('b_coverage')}
3794 summary_info += {'thread sanitizer': config_host.has_key('CONFIG_TSAN')}
3795 summary_info += {'CFI support': get_option('cfi')}
3796 if get_option('cfi')
3797 summary_info += {'CFI debug support': get_option('cfi_debug')}
3799 summary_info += {'strip binaries': get_option('strip')}
3800 summary_info += {'sparse': sparse}
3801 summary_info += {'mingw32 support': targetos == 'windows'}
3802 summary(summary_info, bool_yn: true, section: 'Compilation')
3804 # snarf the cross-compilation information for tests
3807 foreach target: target_dirs
3808 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak'
3809 if fs.exists(tcg_mak)
3810 config_cross_tcg = keyval.load(tcg_mak)
3811 if 'CC' in config_cross_tcg
3812 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']}
3818 summary(summary_info, bool_yn: true, section: 'Cross compilers')
3821 # Targets and accelerators
3824 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')}
3825 summary_info += {'HAX support': config_all.has_key('CONFIG_HAX')}
3826 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')}
3827 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')}
3828 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')}
3829 summary_info += {'Xen support': xen.found()}
3831 summary_info += {'xen ctrl version': xen.version()}
3834 summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')}
3835 if config_all.has_key('CONFIG_TCG')
3836 if get_option('tcg_interpreter')
3837 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'}
3839 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)}
3841 summary_info += {'TCG plugins': config_host.has_key('CONFIG_PLUGIN')}
3842 summary_info += {'TCG debug enabled': config_host.has_key('CONFIG_DEBUG_TCG')}
3844 summary_info += {'target list': ' '.join(target_dirs)}
3846 summary_info += {'default devices': get_option('default_devices')}
3847 summary_info += {'out of process emulation': multiprocess_allowed}
3848 summary_info += {'vfio-user server': vfio_user_server_allowed}
3850 summary(summary_info, bool_yn: true, section: 'Targets and accelerators')
3854 summary_info += {'coroutine backend': config_host['CONFIG_COROUTINE_BACKEND']}
3855 summary_info += {'coroutine pool': have_coroutine_pool}
3857 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')}
3858 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')}
3859 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')}
3860 summary_info += {'VirtFS support': have_virtfs}
3861 summary_info += {'build virtiofs daemon': have_virtiofsd}
3862 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')}
3863 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')}
3864 summary_info += {'bochs support': get_option('bochs').allowed()}
3865 summary_info += {'cloop support': get_option('cloop').allowed()}
3866 summary_info += {'dmg support': get_option('dmg').allowed()}
3867 summary_info += {'qcow v1 support': get_option('qcow1').allowed()}
3868 summary_info += {'vdi support': get_option('vdi').allowed()}
3869 summary_info += {'vvfat support': get_option('vvfat').allowed()}
3870 summary_info += {'qed support': get_option('qed').allowed()}
3871 summary_info += {'parallels support': get_option('parallels').allowed()}
3872 summary_info += {'FUSE exports': fuse}
3873 summary_info += {'VDUSE block exports': have_vduse_blk_export}
3875 summary(summary_info, bool_yn: true, section: 'Block layer support')
3879 summary_info += {'TLS priority': get_option('tls_priority')}
3880 summary_info += {'GNUTLS support': gnutls}
3882 summary_info += {' GNUTLS crypto': gnutls_crypto.found()}
3884 summary_info += {'libgcrypt': gcrypt}
3885 summary_info += {'nettle': nettle}
3887 summary_info += {' XTS': xts != 'private'}
3889 summary_info += {'AF_ALG support': have_afalg}
3890 summary_info += {'rng-none': get_option('rng_none')}
3891 summary_info += {'Linux keyring': have_keyring}
3892 summary(summary_info, bool_yn: true, section: 'Crypto')
3896 if targetos == 'darwin'
3897 summary_info += {'Cocoa support': cocoa}
3898 summary_info += {'vmnet.framework support': vmnet}
3900 summary_info += {'SDL support': sdl}
3901 summary_info += {'SDL image support': sdl_image}
3902 summary_info += {'GTK support': gtk}
3903 summary_info += {'pixman': pixman}
3904 summary_info += {'VTE support': vte}
3905 summary_info += {'slirp support': slirp}
3906 summary_info += {'libtasn1': tasn1}
3907 summary_info += {'PAM': pam}
3908 summary_info += {'iconv support': iconv}
3909 summary_info += {'curses support': curses}
3910 summary_info += {'virgl support': virgl}
3911 summary_info += {'blkio support': blkio}
3912 summary_info += {'curl support': curl}
3913 summary_info += {'Multipath support': mpathpersist}
3914 summary_info += {'PNG support': png}
3915 summary_info += {'VNC support': vnc}
3917 summary_info += {'VNC SASL support': sasl}
3918 summary_info += {'VNC JPEG support': jpeg}
3920 if targetos not in ['darwin', 'haiku', 'windows']
3921 summary_info += {'OSS support': oss}
3922 summary_info += {'sndio support': sndio}
3923 elif targetos == 'darwin'
3924 summary_info += {'CoreAudio support': coreaudio}
3925 elif targetos == 'windows'
3926 summary_info += {'DirectSound support': dsound}
3928 if targetos == 'linux'
3929 summary_info += {'ALSA support': alsa}
3930 summary_info += {'PulseAudio support': pulse}
3932 summary_info += {'JACK support': jack}
3933 summary_info += {'brlapi support': brlapi}
3934 summary_info += {'vde support': vde}
3935 summary_info += {'netmap support': have_netmap}
3936 summary_info += {'l2tpv3 support': have_l2tpv3}
3937 summary_info += {'Linux AIO support': libaio}
3938 summary_info += {'Linux io_uring support': linux_io_uring}
3939 summary_info += {'ATTR/XATTR support': libattr}
3940 summary_info += {'RDMA support': rdma}
3941 summary_info += {'PVRDMA support': have_pvrdma}
3942 summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt}
3943 summary_info += {'libcap-ng support': libcap_ng}
3944 summary_info += {'bpf support': libbpf}
3945 summary_info += {'spice protocol support': spice_protocol}
3946 if spice_protocol.found()
3947 summary_info += {' spice server support': spice}
3949 summary_info += {'rbd support': rbd}
3950 summary_info += {'smartcard support': cacard}
3951 summary_info += {'U2F support': u2f}
3952 summary_info += {'libusb': libusb}
3953 summary_info += {'usb net redir': usbredir}
3954 summary_info += {'OpenGL support (epoxy)': opengl}
3955 summary_info += {'GBM': gbm}
3956 summary_info += {'libiscsi support': libiscsi}
3957 summary_info += {'libnfs support': libnfs}
3958 if targetos == 'windows'
3960 summary_info += {'QGA VSS support': have_qga_vss}
3963 summary_info += {'seccomp support': seccomp}
3964 summary_info += {'GlusterFS support': glusterfs}
3965 summary_info += {'TPM support': have_tpm}
3966 summary_info += {'libssh support': libssh}
3967 summary_info += {'lzo support': lzo}
3968 summary_info += {'snappy support': snappy}
3969 summary_info += {'bzip2 support': libbzip2}
3970 summary_info += {'lzfse support': liblzfse}
3971 summary_info += {'zstd support': zstd}
3972 summary_info += {'NUMA host support': numa}
3973 summary_info += {'capstone': capstone}
3974 summary_info += {'libpmem support': libpmem}
3975 summary_info += {'libdaxctl support': libdaxctl}
3976 summary_info += {'libudev': libudev}
3977 # Dummy dependency, keep .found()
3978 summary_info += {'FUSE lseek': fuse_lseek.found()}
3979 summary_info += {'selinux': selinux}
3980 summary(summary_info, bool_yn: true, section: 'Dependencies')
3982 if not supported_cpus.contains(cpu)
3984 warning('SUPPORT FOR THIS HOST CPU WILL GO AWAY IN FUTURE RELEASES!')
3986 message('CPU host architecture ' + cpu + ' support is not currently maintained.')
3987 message('The QEMU project intends to remove support for this host CPU in')
3988 message('a future release if nobody volunteers to maintain it and to')
3989 message('provide a build host for our continuous integration setup.')
3990 message('configure has succeeded and you can continue to build, but')
3991 message('if you care about QEMU on this platform you should contact')
3992 message('us upstream at qemu-devel@nongnu.org.')
3995 if not supported_oses.contains(targetos)
3997 warning('WARNING: SUPPORT FOR THIS HOST OS WILL GO AWAY IN FUTURE RELEASES!')
3999 message('Host OS ' + targetos + 'support is not currently maintained.')
4000 message('The QEMU project intends to remove support for this host OS in')
4001 message('a future release if nobody volunteers to maintain it and to')
4002 message('provide a build host for our continuous integration setup.')
4003 message('configure has succeeded and you can continue to build, but')
4004 message('if you care about QEMU on this platform you should contact')
4005 message('us upstream at qemu-devel@nongnu.org.')