1 project('qemu', ['c'], meson_version: '>=0.61.3',
2 default_options: ['warning_level=1', 'c_std=gnu11', 'cpp_std=gnu++11', 'b_colorout=auto',
3 'b_staticpic=false', 'stdsplit=false', 'optimization=2', 'b_pie=true'],
4 version: files('VERSION'))
6 add_test_setup('quick', exclude_suites: ['slow', 'thorough'], is_default: true)
7 add_test_setup('slow', exclude_suites: ['thorough'], env: ['G_TEST_SLOW=1', 'SPEED=slow'])
8 add_test_setup('thorough', env: ['G_TEST_SLOW=1', 'SPEED=thorough'])
10 meson.add_postconf_script(find_program('scripts/symlink-install-tree.py'))
12 not_found = dependency('', required: false)
13 keyval = import('keyval')
14 ss = import('sourceset')
17 targetos = host_machine.system()
18 sh = find_program('sh')
19 config_host = keyval.load(meson.current_build_dir() / 'config-host.mak')
20 enable_modules = 'CONFIG_MODULES' in config_host
21 enable_static = 'CONFIG_STATIC' in config_host
23 # Allow both shared and static libraries unless --enable-static
24 static_kwargs = enable_static ? {'static': true} : {}
26 cc = meson.get_compiler('c')
28 if add_languages('cpp', required: false, native: false)
29 all_languages += ['cpp']
30 cxx = meson.get_compiler('cpp')
32 if targetos == 'darwin' and \
33 add_languages('objc', required: get_option('cocoa'), native: false)
34 all_languages += ['objc']
35 objc = meson.get_compiler('objc')
38 # Temporary directory used for files created while
39 # configure runs. Since it is in the build directory
40 # we can safely blow away any previous version of it
41 # (and we need not jump through hoops to try to delete
42 # it when configure exits.)
43 tmpdir = meson.current_build_dir() / 'meson-private/temp'
45 if get_option('qemu_suffix').startswith('/')
46 error('qemu_suffix cannot start with a /')
49 qemu_confdir = get_option('sysconfdir') / get_option('qemu_suffix')
50 qemu_datadir = get_option('datadir') / get_option('qemu_suffix')
51 qemu_docdir = get_option('docdir') / get_option('qemu_suffix')
52 qemu_moddir = get_option('libdir') / get_option('qemu_suffix')
54 qemu_desktopdir = get_option('datadir') / 'applications'
55 qemu_icondir = get_option('datadir') / 'icons'
57 config_host_data = configuration_data()
59 qapi_trace_events = []
61 bsd_oses = ['gnu/kfreebsd', 'freebsd', 'netbsd', 'openbsd', 'dragonfly', 'darwin']
62 supported_oses = ['windows', 'freebsd', 'netbsd', 'openbsd', 'darwin', 'sunos', 'linux']
63 supported_cpus = ['ppc', 'ppc64', 's390x', 'riscv', 'x86', 'x86_64',
64 'arm', 'aarch64', 'loongarch64', 'mips', 'mips64', 'sparc64']
66 cpu = host_machine.cpu_family()
68 # Unify riscv* to a single family.
69 if cpu in ['riscv32', 'riscv64']
73 target_dirs = config_host['TARGET_DIRS'].split()
74 have_linux_user = false
77 foreach target : target_dirs
78 have_linux_user = have_linux_user or target.endswith('linux-user')
79 have_bsd_user = have_bsd_user or target.endswith('bsd-user')
80 have_system = have_system or target.endswith('-softmmu')
82 have_user = have_linux_user or have_bsd_user
83 have_tools = get_option('tools') \
84 .disable_auto_if(not have_system) \
86 have_ga = get_option('guest_agent') \
87 .disable_auto_if(not have_system and not have_tools) \
88 .require(targetos in ['sunos', 'linux', 'windows', 'freebsd', 'netbsd', 'openbsd'],
89 error_message: 'unsupported OS for QEMU guest agent') \
91 have_block = have_system or have_tools
93 python = import('python').find_installation()
95 if cpu not in supported_cpus
105 if cpu in ['x86', 'x86_64']
106 kvm_targets = ['i386-softmmu', 'x86_64-softmmu']
107 elif cpu == 'aarch64'
108 kvm_targets = ['aarch64-softmmu']
110 kvm_targets = ['s390x-softmmu']
111 elif cpu in ['ppc', 'ppc64']
112 kvm_targets = ['ppc-softmmu', 'ppc64-softmmu']
113 elif cpu in ['mips', 'mips64']
114 kvm_targets = ['mips-softmmu', 'mipsel-softmmu', 'mips64-softmmu', 'mips64el-softmmu']
115 elif cpu in ['riscv']
116 kvm_targets = ['riscv32-softmmu', 'riscv64-softmmu']
122 if get_option('kvm').allowed() and targetos == 'linux'
123 kvm_targets_c = '"' + '" ,"'.join(kvm_targets) + '"'
125 config_host_data.set('CONFIG_KVM_TARGETS', kvm_targets_c)
127 accelerator_targets = { 'CONFIG_KVM': kvm_targets }
129 if cpu in ['aarch64']
130 accelerator_targets += {
131 'CONFIG_HVF': ['aarch64-softmmu']
135 if cpu in ['x86', 'x86_64', 'arm', 'aarch64']
136 # i386 emulator provides xenpv machine type for multiple architectures
137 accelerator_targets += {
138 'CONFIG_XEN': ['i386-softmmu', 'x86_64-softmmu'],
141 if cpu in ['x86', 'x86_64']
142 accelerator_targets += {
143 'CONFIG_HAX': ['i386-softmmu', 'x86_64-softmmu'],
144 'CONFIG_HVF': ['x86_64-softmmu'],
145 'CONFIG_NVMM': ['i386-softmmu', 'x86_64-softmmu'],
146 'CONFIG_WHPX': ['i386-softmmu', 'x86_64-softmmu'],
151 # Darwin does not support references to thread-local variables in modules
152 if targetos != 'darwin'
153 modular_tcg = ['i386-softmmu', 'x86_64-softmmu']
156 edk2_targets = [ 'arm-softmmu', 'aarch64-softmmu', 'i386-softmmu', 'x86_64-softmmu' ]
157 unpack_edk2_blobs = false
158 foreach target : edk2_targets
159 if target in target_dirs
160 bzip2 = find_program('bzip2', required: get_option('install_blobs'))
161 unpack_edk2_blobs = bzip2.found()
168 if 'dtrace' in get_option('trace_backends')
169 dtrace = find_program('dtrace', required: true)
170 stap = find_program('stap', required: false)
172 # Workaround to avoid dtrace(1) producing a file with 'hidden' symbol
173 # visibility. Define STAP_SDT_V2 to produce 'default' symbol visibility
174 # instead. QEMU --enable-modules depends on this because the SystemTap
175 # semaphores are linked into the main binary and not the module's shared
177 add_global_arguments('-DSTAP_SDT_V2',
178 native: false, language: all_languages)
182 if get_option('iasl') == ''
183 iasl = find_program('iasl', required: false)
185 iasl = find_program(get_option('iasl'), required: true)
192 qemu_cflags = config_host['QEMU_CFLAGS'].split()
193 qemu_objcflags = config_host['QEMU_OBJCFLAGS'].split()
194 qemu_ldflags = config_host['QEMU_LDFLAGS'].split()
197 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static'
200 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
201 # The combination is known as "full relro", because .got.plt is read-only too.
202 qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now')
204 if targetos == 'windows'
205 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--no-seh', '-Wl,--nxcompat')
206 qemu_ldflags += cc.get_supported_link_arguments('-Wl,--dynamicbase', '-Wl,--high-entropy-va')
209 if get_option('gprof')
210 qemu_cflags += ['-p']
211 qemu_objcflags += ['-p']
212 qemu_ldflags += ['-p']
215 # Specify linker-script with add_project_link_arguments so that it is not placed
216 # within a linker --start-group/--end-group pair
217 if get_option('fuzzing')
218 # Specify a filter to only instrument code that is directly related to
220 configure_file(output: 'instrumentation-filter',
221 input: 'scripts/oss-fuzz/instrumentation-filter-template',
224 if cc.compiles('int main () { return 0; }',
225 name: '-fsanitize-coverage-allowlist=/dev/null',
226 args: ['-fsanitize-coverage-allowlist=/dev/null',
227 '-fsanitize-coverage=trace-pc'] )
228 add_global_arguments('-fsanitize-coverage-allowlist=instrumentation-filter',
229 native: false, language: all_languages)
232 if get_option('fuzzing_engine') == ''
233 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the
234 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link
235 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be
236 # unable to bind the fuzzer-related callbacks added by instrumentation.
237 add_global_arguments('-fsanitize=fuzzer-no-link',
238 native: false, language: all_languages)
239 add_global_link_arguments('-fsanitize=fuzzer-no-link',
240 native: false, language: all_languages)
241 # For the actual fuzzer binaries, we need to link against the libfuzzer
242 # library. They need to be configurable, to support OSS-Fuzz
243 fuzz_exe_ldflags = ['-fsanitize=fuzzer']
245 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and
246 # the needed CFLAGS have already been provided
247 fuzz_exe_ldflags = get_option('fuzzing_engine').split()
251 # Check that the C++ compiler exists and works with the C compiler.
255 if 'cpp' in all_languages
256 add_global_arguments(['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'],
257 native: false, language: 'cpp')
258 foreach k: qemu_cflags
259 if k not in ['-Wstrict-prototypes', '-Wmissing-prototypes', '-Wnested-externs',
260 '-Wold-style-declaration', '-Wold-style-definition', '-Wredundant-decls']
265 if cxx.links(files('scripts/main.c'), args: qemu_cflags)
266 link_language = 'cpp'
269 message('C++ compiler does not work with C compiler')
270 message('Disabling C++-specific optional code')
274 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
275 if targetos != 'sunos' and not config_host.has_key('CONFIG_TSAN')
276 qemu_ldflags += linker.get_supported_link_arguments('-Wl,--warn-common')
279 add_global_link_arguments(qemu_ldflags, native: false, language: all_languages)
281 add_global_arguments(qemu_cflags, native: false, language: 'c')
282 add_global_arguments(qemu_cxxflags, native: false, language: 'cpp')
283 add_global_arguments(qemu_objcflags, native: false, language: 'objc')
284 if targetos == 'linux'
285 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers',
286 '-isystem', 'linux-headers',
287 language: all_languages)
290 add_project_arguments('-iquote', '.',
291 '-iquote', meson.current_source_dir(),
292 '-iquote', meson.current_source_dir() / 'include',
293 language: all_languages)
295 sparse = find_program('cgcc', required: get_option('sparse'))
298 command: [find_program('scripts/check_sparse.py'),
299 'compile_commands.json', sparse.full_path(), '-Wbitwise',
300 '-Wno-transparent-union', '-Wno-old-initializer',
301 '-Wno-non-pointer-null'])
304 ###########################################
305 # Target-specific checks and dependencies #
306 ###########################################
309 if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \
312 #include <sys/types.h>
313 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
314 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
316 args: ['-Werror', '-fsanitize=fuzzer'])
317 error('Your compiler does not support -fsanitize=fuzzer')
321 if 'ftrace' in get_option('trace_backends') and targetos != 'linux'
322 error('ftrace is supported only on Linux')
324 if 'syslog' in get_option('trace_backends') and not cc.compiles('''
327 openlog("qemu", LOG_PID, LOG_DAEMON);
328 syslog(LOG_INFO, "configure");
331 error('syslog is not supported on this system')
334 # Miscellaneous Linux-only features
335 get_option('mpath') \
336 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux')
338 multiprocess_allowed = get_option('multiprocess') \
339 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \
342 vfio_user_server_allowed = get_option('vfio_user_server') \
343 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \
346 have_tpm = get_option('tpm') \
347 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \
351 have_vhost_user = get_option('vhost_user') \
352 .disable_auto_if(targetos != 'linux') \
353 .require(targetos != 'windows',
354 error_message: 'vhost-user is not available on Windows').allowed()
355 have_vhost_vdpa = get_option('vhost_vdpa') \
356 .require(targetos == 'linux',
357 error_message: 'vhost-vdpa is only available on Linux').allowed()
358 have_vhost_kernel = get_option('vhost_kernel') \
359 .require(targetos == 'linux',
360 error_message: 'vhost-kernel is only available on Linux').allowed()
361 have_vhost_user_crypto = get_option('vhost_crypto') \
362 .require(have_vhost_user,
363 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed()
365 have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel
367 have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed()
368 have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed()
369 have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed()
370 have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa
372 # Target-specific libraries and flags
373 libm = cc.find_library('m', required: false)
374 threads = dependency('threads')
375 util = cc.find_library('util', required: false)
381 emulator_link_args = []
388 if targetos == 'windows'
389 midl = find_program('midl', required: false)
390 widl = find_program('widl', required: false)
391 pathcch = cc.find_library('pathcch')
392 socket = cc.find_library('ws2_32')
393 winmm = cc.find_library('winmm')
395 win = import('windows')
396 version_res = win.compile_resources('version.rc',
397 depend_files: files('pc-bios/qemu-nsis.ico'),
398 include_directories: include_directories('.'))
400 elif targetos == 'darwin'
401 coref = dependency('appleframeworks', modules: 'CoreFoundation')
402 iokit = dependency('appleframeworks', modules: 'IOKit', required: false)
403 host_dsosuf = '.dylib'
404 elif targetos == 'sunos'
405 socket = [cc.find_library('socket'),
406 cc.find_library('nsl'),
407 cc.find_library('resolv')]
408 elif targetos == 'haiku'
409 socket = [cc.find_library('posix_error_mapper'),
410 cc.find_library('network'),
411 cc.find_library('bsd')]
412 elif targetos == 'openbsd'
413 if get_option('tcg').allowed() and target_dirs.length() > 0
414 # Disable OpenBSD W^X if available
415 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded')
419 # Target-specific configuration of accelerators
421 if get_option('kvm').allowed() and targetos == 'linux'
422 accelerators += 'CONFIG_KVM'
424 if get_option('whpx').allowed() and targetos == 'windows'
425 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64'
426 error('WHPX requires 64-bit host')
427 elif cc.has_header('WinHvPlatform.h', required: get_option('whpx')) and \
428 cc.has_header('WinHvEmulation.h', required: get_option('whpx'))
429 accelerators += 'CONFIG_WHPX'
432 if get_option('hvf').allowed()
433 hvf = dependency('appleframeworks', modules: 'Hypervisor',
434 required: get_option('hvf'))
436 accelerators += 'CONFIG_HVF'
439 if get_option('hax').allowed()
440 if get_option('hax').enabled() or targetos in ['windows', 'darwin', 'netbsd']
441 accelerators += 'CONFIG_HAX'
444 if targetos == 'netbsd'
445 nvmm = cc.find_library('nvmm', required: get_option('nvmm'))
447 accelerators += 'CONFIG_NVMM'
452 if get_option('tcg').allowed()
453 if host_arch == 'unknown'
454 if get_option('tcg_interpreter')
455 warning('Unsupported CPU @0@, will use TCG with TCI (slow)'.format(cpu))
457 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu))
459 elif get_option('tcg_interpreter')
460 warning('Use of the TCG interpreter is not recommended on this host')
461 warning('architecture. There is a native TCG execution backend available')
462 warning('which provides substantially better performance and reliability.')
463 warning('It is strongly recommended to remove the --enable-tcg-interpreter')
464 warning('configuration option on this architecture to use the native')
467 if get_option('tcg_interpreter')
469 config_host += { 'CONFIG_TCG_INTERPRETER': 'y' }
470 elif host_arch == 'x86_64'
472 elif host_arch == 'ppc64'
475 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch,
476 language: all_languages)
478 accelerators += 'CONFIG_TCG'
479 config_host += { 'CONFIG_TCG': 'y' }
482 if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled()
483 error('KVM not available on this platform')
485 if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled()
486 error('HVF not available on this platform')
488 if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled()
489 error('NVMM not available on this platform')
491 if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled()
492 error('WHPX not available on this platform')
499 # The path to glib.h is added to all compilation commands. This was
500 # grandfathered in from the QEMU Makefiles.
501 add_project_arguments(config_host['GLIB_CFLAGS'].split(),
502 native: false, language: all_languages)
503 glib = declare_dependency(compile_args: config_host['GLIB_CFLAGS'].split(),
504 link_args: config_host['GLIB_LIBS'].split(),
505 version: config_host['GLIB_VERSION'],
507 'bindir': config_host['GLIB_BINDIR'],
509 # override glib dep with the configure results (for subprojects)
510 meson.override_dependency('glib-2.0', glib)
513 gdbus_codegen = not_found
514 gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio'
515 if not get_option('gio').auto() or have_system
516 gio = dependency('gio-2.0', required: get_option('gio'),
517 method: 'pkg-config', kwargs: static_kwargs)
518 if gio.found() and not cc.links('''
522 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
524 }''', dependencies: [glib, gio])
525 if get_option('gio').enabled()
526 error('The installed libgio is broken for static linking')
531 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'),
532 required: get_option('gio'))
533 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'),
534 method: 'pkg-config', kwargs: static_kwargs)
535 gio = declare_dependency(dependencies: [gio, gio_unix],
536 version: gio.version())
539 if gdbus_codegen.found() and get_option('cfi')
540 gdbus_codegen = not_found
541 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity'
545 if 'ust' in get_option('trace_backends')
546 lttng = dependency('lttng-ust', required: true, version: '>= 2.1',
547 method: 'pkg-config', kwargs: static_kwargs)
550 if have_system or have_tools
551 pixman = dependency('pixman-1', required: have_system, version:'>=0.21.8',
552 method: 'pkg-config', kwargs: static_kwargs)
554 zlib = dependency('zlib', required: true, kwargs: static_kwargs)
557 if not get_option('linux_aio').auto() or have_block
558 libaio = cc.find_library('aio', has_headers: ['libaio.h'],
559 required: get_option('linux_aio'),
560 kwargs: static_kwargs)
563 linux_io_uring_test = '''
564 #include <liburing.h>
565 #include <linux/errqueue.h>
567 int main(void) { return 0; }'''
569 linux_io_uring = not_found
570 if not get_option('linux_io_uring').auto() or have_block
571 linux_io_uring = dependency('liburing', version: '>=0.3',
572 required: get_option('linux_io_uring'),
573 method: 'pkg-config', kwargs: static_kwargs)
574 if not cc.links(linux_io_uring_test)
575 linux_io_uring = not_found
580 if not get_option('libnfs').auto() or have_block
581 libnfs = dependency('libnfs', version: '>=1.9.3',
582 required: get_option('libnfs'),
583 method: 'pkg-config', kwargs: static_kwargs)
588 #include <sys/types.h>
589 #ifdef CONFIG_LIBATTR
590 #include <attr/xattr.h>
592 #include <sys/xattr.h>
594 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }'''
597 have_old_libattr = false
598 if get_option('attr').allowed()
599 if cc.links(libattr_test)
600 libattr = declare_dependency()
602 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'],
603 required: get_option('attr'),
604 kwargs: static_kwargs)
605 if libattr.found() and not \
606 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR')
608 if get_option('attr').enabled()
609 error('could not link libattr')
611 warning('could not link libattr, disabling')
614 have_old_libattr = libattr.found()
619 cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'],
620 required: get_option('cocoa'))
622 vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet'))
623 if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h',
624 'VMNET_BRIDGED_MODE',
627 if get_option('vmnet').enabled()
628 error('vmnet.framework API is outdated')
630 warning('vmnet.framework API is outdated, disabling')
635 seccomp_has_sysrawrc = false
636 if not get_option('seccomp').auto() or have_system or have_tools
637 seccomp = dependency('libseccomp', version: '>=2.3.0',
638 required: get_option('seccomp'),
639 method: 'pkg-config', kwargs: static_kwargs)
641 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h',
642 'SCMP_FLTATR_API_SYSRAWRC',
643 dependencies: seccomp)
647 libcap_ng = not_found
648 if not get_option('cap_ng').auto() or have_system or have_tools
649 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'],
650 required: get_option('cap_ng'),
651 kwargs: static_kwargs)
653 if libcap_ng.found() and not cc.links('''
657 capng_capability_to_name(CAPNG_EFFECTIVE);
659 }''', dependencies: libcap_ng)
660 libcap_ng = not_found
661 if get_option('cap_ng').enabled()
662 error('could not link libcap-ng')
664 warning('could not link libcap-ng, disabling')
668 if get_option('xkbcommon').auto() and not have_system and not have_tools
669 xkbcommon = not_found
671 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'),
672 method: 'pkg-config', kwargs: static_kwargs)
676 if not get_option('slirp').auto() or have_system
677 slirp = dependency('slirp', required: get_option('slirp'),
678 method: 'pkg-config', kwargs: static_kwargs)
679 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because
680 # it passes function pointers within libslirp as callbacks for timers.
681 # When using a system-wide shared libslirp, the type information for the
682 # callback is missing and the timer call produces a false positive with CFI.
683 # Do not use the "version" keyword argument to produce a better error.
684 # with control-flow integrity.
685 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7')
686 if get_option('slirp').enabled()
687 error('Control-Flow Integrity requires libslirp 4.7.')
689 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.')
696 if not get_option('vde').auto() or have_system or have_tools
697 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'],
698 required: get_option('vde'),
699 kwargs: static_kwargs)
701 if vde.found() and not cc.links('''
702 #include <libvdeplug.h>
705 struct vde_open_args a = {0, 0, 0};
709 }''', dependencies: vde)
711 if get_option('cap_ng').enabled()
712 error('could not link libvdeplug')
714 warning('could not link libvdeplug, disabling')
719 if not get_option('pa').auto() or (targetos == 'linux' and have_system)
720 pulse = dependency('libpulse', required: get_option('pa'),
721 method: 'pkg-config', kwargs: static_kwargs)
724 if not get_option('alsa').auto() or (targetos == 'linux' and have_system)
725 alsa = dependency('alsa', required: get_option('alsa'),
726 method: 'pkg-config', kwargs: static_kwargs)
729 if not get_option('jack').auto() or have_system
730 jack = dependency('jack', required: get_option('jack'),
731 method: 'pkg-config', kwargs: static_kwargs)
734 if not get_option('sndio').auto() or have_system
735 sndio = dependency('sndio', required: get_option('sndio'),
736 method: 'pkg-config', kwargs: static_kwargs)
739 spice_protocol = not_found
740 if not get_option('spice_protocol').auto() or have_system
741 spice_protocol = dependency('spice-protocol', version: '>=0.14.0',
742 required: get_option('spice_protocol'),
743 method: 'pkg-config', kwargs: static_kwargs)
746 if not get_option('spice').auto() or have_system
747 spice = dependency('spice-server', version: '>=0.14.0',
748 required: get_option('spice'),
749 method: 'pkg-config', kwargs: static_kwargs)
751 spice_headers = spice.partial_dependency(compile_args: true, includes: true)
753 rt = cc.find_library('rt', required: false)
756 if not get_option('libiscsi').auto() or have_block
757 libiscsi = dependency('libiscsi', version: '>=1.9.0',
758 required: get_option('libiscsi'),
759 method: 'pkg-config', kwargs: static_kwargs)
762 if not get_option('zstd').auto() or have_block
763 zstd = dependency('libzstd', version: '>=1.4.0',
764 required: get_option('zstd'),
765 method: 'pkg-config', kwargs: static_kwargs)
769 have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found()
770 if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu
771 virgl = dependency('virglrenderer',
772 method: 'pkg-config',
773 required: get_option('virglrenderer'),
774 kwargs: static_kwargs)
777 if not get_option('blkio').auto() or have_block
778 blkio = dependency('blkio',
779 method: 'pkg-config',
780 required: get_option('blkio'),
781 kwargs: static_kwargs)
784 if not get_option('curl').auto() or have_block
785 curl = dependency('libcurl', version: '>=7.29.0',
786 method: 'pkg-config',
787 required: get_option('curl'),
788 kwargs: static_kwargs)
791 if targetos == 'linux' and (have_system or have_tools)
792 libudev = dependency('libudev',
793 method: 'pkg-config',
794 required: get_option('libudev'),
795 kwargs: static_kwargs)
798 mpathlibs = [libudev]
799 mpathpersist = not_found
800 mpathpersist_new_api = false
801 if targetos == 'linux' and have_tools and get_option('mpath').allowed()
802 mpath_test_source_new = '''
804 #include <mpath_persist.h>
805 unsigned mpath_mx_alloc_len = 1024;
807 static struct config *multipath_conf;
808 extern struct udev *udev;
809 extern struct config *get_multipath_config(void);
810 extern void put_multipath_config(struct config *conf);
812 struct config *get_multipath_config(void) { return multipath_conf; }
813 void put_multipath_config(struct config *conf) { }
816 multipath_conf = mpath_lib_init();
819 mpath_test_source_old = '''
821 #include <mpath_persist.h>
822 unsigned mpath_mx_alloc_len = 1024;
825 struct udev *udev = udev_new();
826 mpath_lib_init(udev);
829 libmpathpersist = cc.find_library('mpathpersist',
830 required: get_option('mpath'),
831 kwargs: static_kwargs)
832 if libmpathpersist.found()
833 mpathlibs += libmpathpersist
835 mpathlibs += cc.find_library('devmapper',
836 required: get_option('mpath'),
837 kwargs: static_kwargs)
839 mpathlibs += cc.find_library('multipath',
840 required: get_option('mpath'),
841 kwargs: static_kwargs)
842 foreach lib: mpathlibs
848 if mpathlibs.length() == 0
849 msg = 'Dependencies missing for libmpathpersist'
850 elif cc.links(mpath_test_source_new, dependencies: mpathlibs)
851 mpathpersist = declare_dependency(dependencies: mpathlibs)
852 mpathpersist_new_api = true
853 elif cc.links(mpath_test_source_old, dependencies: mpathlibs)
854 mpathpersist = declare_dependency(dependencies: mpathlibs)
856 msg = 'Cannot detect libmpathpersist API'
858 if not mpathpersist.found()
859 if get_option('mpath').enabled()
862 warning(msg + ', disabling')
870 if have_system and get_option('curses').allowed()
872 #if defined(__APPLE__) || defined(__OpenBSD__)
873 #define _XOPEN_SOURCE_EXTENDED 1
880 setlocale(LC_ALL, "");
882 addwstr(L"wide chars\n");
884 add_wch(WACS_DEGREE);
888 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw']
889 curses = dependency(curses_dep_list,
891 method: 'pkg-config',
892 kwargs: static_kwargs)
893 msg = get_option('curses').enabled() ? 'curses library not found' : ''
894 curses_compile_args = ['-DNCURSES_WIDECHAR=1']
896 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses])
897 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses])
899 msg = 'curses package not usable'
903 if not curses.found()
904 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
905 if targetos != 'windows' and not has_curses_h
906 message('Trying with /usr/include/ncursesw')
907 curses_compile_args += ['-I/usr/include/ncursesw']
908 has_curses_h = cc.has_header('curses.h', args: curses_compile_args)
911 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw'])
912 foreach curses_libname : curses_libname_list
913 libcurses = cc.find_library(curses_libname,
915 kwargs: static_kwargs)
917 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses)
918 curses = declare_dependency(compile_args: curses_compile_args,
919 dependencies: [libcurses])
922 msg = 'curses library not usable'
928 if get_option('iconv').allowed()
929 foreach link_args : [ ['-liconv'], [] ]
930 # Programs will be linked with glib and this will bring in libiconv on FreeBSD.
931 # We need to use libiconv if available because mixing libiconv's headers with
932 # the system libc does not work.
933 # However, without adding glib to the dependencies -L/usr/local/lib will not be
934 # included in the command line and libiconv will not be found.
938 iconv_t conv = iconv_open("WCHAR_T", "UCS-2");
939 return conv != (iconv_t) -1;
940 }''', args: config_host['GLIB_CFLAGS'].split() + config_host['GLIB_LIBS'].split() + link_args)
941 iconv = declare_dependency(link_args: link_args, dependencies: glib)
946 if curses.found() and not iconv.found()
947 if get_option('iconv').enabled()
948 error('iconv not available')
950 msg = 'iconv required for curses UI but not available'
953 if not curses.found() and msg != ''
954 if get_option('curses').enabled()
957 warning(msg + ', disabling')
963 if not get_option('brlapi').auto() or have_system
964 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'],
965 required: get_option('brlapi'),
966 kwargs: static_kwargs)
967 if brlapi.found() and not cc.links('''
970 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi)
972 if get_option('brlapi').enabled()
973 error('could not link brlapi')
975 warning('could not link brlapi, disabling')
981 if not get_option('sdl').auto() or have_system
982 sdl = dependency('sdl2', required: get_option('sdl'), kwargs: static_kwargs)
983 sdl_image = not_found
986 # work around 2.0.8 bug
987 sdl = declare_dependency(compile_args: '-Wno-undef',
989 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'),
990 method: 'pkg-config', kwargs: static_kwargs)
992 if get_option('sdl_image').enabled()
993 error('sdl-image required, but SDL was @0@'.format(
994 get_option('sdl').disabled() ? 'disabled' : 'not found'))
996 sdl_image = not_found
1000 if not get_option('rbd').auto() or have_block
1001 librados = cc.find_library('rados', required: get_option('rbd'),
1002 kwargs: static_kwargs)
1003 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'],
1004 required: get_option('rbd'),
1005 kwargs: static_kwargs)
1006 if librados.found() and librbd.found()
1009 #include <rbd/librbd.h>
1012 rados_create(&cluster, NULL);
1013 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0)
1017 }''', dependencies: [librbd, librados])
1018 rbd = declare_dependency(dependencies: [librbd, librados])
1019 elif get_option('rbd').enabled()
1020 error('librbd >= 1.12.0 required')
1022 warning('librbd >= 1.12.0 not found, disabling')
1027 glusterfs = not_found
1028 glusterfs_ftruncate_has_stat = false
1029 glusterfs_iocb_has_stat = false
1030 if not get_option('glusterfs').auto() or have_block
1031 glusterfs = dependency('glusterfs-api', version: '>=3',
1032 required: get_option('glusterfs'),
1033 method: 'pkg-config', kwargs: static_kwargs)
1034 if glusterfs.found()
1035 glusterfs_ftruncate_has_stat = cc.links('''
1036 #include <glusterfs/api/glfs.h>
1041 /* new glfs_ftruncate() passes two additional args */
1042 return glfs_ftruncate(NULL, 0, NULL, NULL);
1044 ''', dependencies: glusterfs)
1045 glusterfs_iocb_has_stat = cc.links('''
1046 #include <glusterfs/api/glfs.h>
1048 /* new glfs_io_cbk() passes two additional glfs_stat structs */
1050 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
1056 glfs_io_cbk iocb = &glusterfs_iocb;
1057 iocb(NULL, 0 , NULL, NULL, NULL);
1060 ''', dependencies: glusterfs)
1065 if not get_option('libssh').auto() or have_block
1066 libssh = dependency('libssh', version: '>=0.8.7',
1067 method: 'pkg-config',
1068 required: get_option('libssh'),
1069 kwargs: static_kwargs)
1072 libbzip2 = not_found
1073 if not get_option('bzip2').auto() or have_block
1074 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'],
1075 required: get_option('bzip2'),
1076 kwargs: static_kwargs)
1077 if libbzip2.found() and not cc.links('''
1079 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2)
1080 libbzip2 = not_found
1081 if get_option('bzip2').enabled()
1082 error('could not link libbzip2')
1084 warning('could not link libbzip2, disabling')
1089 liblzfse = not_found
1090 if not get_option('lzfse').auto() or have_block
1091 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'],
1092 required: get_option('lzfse'),
1093 kwargs: static_kwargs)
1095 if liblzfse.found() and not cc.links('''
1097 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse)
1098 liblzfse = not_found
1099 if get_option('lzfse').enabled()
1100 error('could not link liblzfse')
1102 warning('could not link liblzfse, disabling')
1107 if get_option('oss').allowed() and have_system
1108 if not cc.has_header('sys/soundcard.h')
1110 elif targetos == 'netbsd'
1111 oss = cc.find_library('ossaudio', required: get_option('oss'),
1112 kwargs: static_kwargs)
1114 oss = declare_dependency()
1118 if get_option('oss').enabled()
1119 error('OSS not found')
1124 if not get_option('dsound').auto() or (targetos == 'windows' and have_system)
1125 if cc.has_header('dsound.h')
1126 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid'])
1129 if not dsound.found()
1130 if get_option('dsound').enabled()
1131 error('DirectSound not found')
1136 coreaudio = not_found
1137 if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system)
1138 coreaudio = dependency('appleframeworks', modules: 'CoreAudio',
1139 required: get_option('coreaudio'))
1143 if not get_option('opengl').auto() or have_system or have_vhost_user_gpu
1144 epoxy = dependency('epoxy', method: 'pkg-config',
1145 required: get_option('opengl'), kwargs: static_kwargs)
1146 if cc.has_header('epoxy/egl.h', dependencies: epoxy)
1148 elif get_option('opengl').enabled()
1149 error('epoxy/egl.h not found')
1153 if (have_system or have_tools) and (virgl.found() or opengl.found())
1154 gbm = dependency('gbm', method: 'pkg-config', required: false,
1155 kwargs: static_kwargs)
1157 have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found()
1160 gnutls_crypto = not_found
1161 if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system)
1162 # For general TLS support our min gnutls matches
1163 # that implied by our platform support matrix
1165 # For the crypto backends, we look for a newer
1168 # Version 3.6.8 is needed to get XTS
1169 # Version 3.6.13 is needed to get PBKDF
1170 # Version 3.6.14 is needed to get HW accelerated XTS
1172 # If newer enough gnutls isn't available, we can
1173 # still use a different crypto backend to satisfy
1174 # the platform support requirements
1175 gnutls_crypto = dependency('gnutls', version: '>=3.6.14',
1176 method: 'pkg-config',
1178 kwargs: static_kwargs)
1179 if gnutls_crypto.found()
1180 gnutls = gnutls_crypto
1182 # Our min version if all we need is TLS
1183 gnutls = dependency('gnutls', version: '>=3.5.18',
1184 method: 'pkg-config',
1185 required: get_option('gnutls'),
1186 kwargs: static_kwargs)
1190 # We prefer use of gnutls for crypto, unless the options
1191 # explicitly asked for nettle or gcrypt.
1193 # If gnutls isn't available for crypto, then we'll prefer
1194 # gcrypt over nettle for performance reasons.
1200 if get_option('nettle').enabled() and get_option('gcrypt').enabled()
1201 error('Only one of gcrypt & nettle can be enabled')
1204 # Explicit nettle/gcrypt request, so ignore gnutls for crypto
1205 if get_option('nettle').enabled() or get_option('gcrypt').enabled()
1206 gnutls_crypto = not_found
1209 if not gnutls_crypto.found()
1210 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled()
1211 gcrypt = dependency('libgcrypt', version: '>=1.8',
1212 method: 'config-tool',
1213 required: get_option('gcrypt'),
1214 kwargs: static_kwargs)
1215 # Debian has removed -lgpg-error from libgcrypt-config
1216 # as it "spreads unnecessary dependencies" which in
1217 # turn breaks static builds...
1218 if gcrypt.found() and enable_static
1219 gcrypt = declare_dependency(dependencies: [
1221 cc.find_library('gpg-error', required: true, kwargs: static_kwargs)])
1224 if (not get_option('nettle').auto() or have_system) and not gcrypt.found()
1225 nettle = dependency('nettle', version: '>=3.4',
1226 method: 'pkg-config',
1227 required: get_option('nettle'),
1228 kwargs: static_kwargs)
1229 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle)
1235 gmp = dependency('gmp', required: false, method: 'pkg-config', kwargs: static_kwargs)
1236 if nettle.found() and gmp.found()
1237 hogweed = dependency('hogweed', version: '>=3.4',
1238 method: 'pkg-config',
1239 required: get_option('nettle'),
1240 kwargs: static_kwargs)
1247 have_gtk_clipboard = get_option('gtk_clipboard').enabled()
1249 if not get_option('gtk').auto() or have_system
1250 gtk = dependency('gtk+-3.0', version: '>=3.22.0',
1251 method: 'pkg-config',
1252 required: get_option('gtk'),
1253 kwargs: static_kwargs)
1255 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0',
1256 method: 'pkg-config',
1258 kwargs: static_kwargs)
1259 gtk = declare_dependency(dependencies: [gtk, gtkx11])
1261 if not get_option('vte').auto() or have_system
1262 vte = dependency('vte-2.91',
1263 method: 'pkg-config',
1264 required: get_option('vte'),
1265 kwargs: static_kwargs)
1267 elif have_gtk_clipboard
1268 error('GTK clipboard requested, but GTK not found')
1274 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found(),
1275 kwargs: static_kwargs)
1278 if get_option('png').allowed() and have_system
1279 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'),
1280 method: 'pkg-config', kwargs: static_kwargs)
1285 if get_option('vnc').allowed() and have_system
1286 vnc = declare_dependency() # dummy dependency
1287 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'),
1288 method: 'pkg-config', kwargs: static_kwargs)
1289 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'],
1290 required: get_option('vnc_sasl'),
1291 kwargs: static_kwargs)
1293 sasl = declare_dependency(dependencies: sasl,
1294 compile_args: '-DSTRUCT_IOVEC_DEFINED')
1299 if not get_option('auth_pam').auto() or have_system
1300 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'],
1301 required: get_option('auth_pam'),
1302 kwargs: static_kwargs)
1304 if pam.found() and not cc.links('''
1306 #include <security/pam_appl.h>
1308 const char *service_name = "qemu";
1309 const char *user = "frank";
1310 const struct pam_conv pam_conv = { 0 };
1311 pam_handle_t *pamh = NULL;
1312 pam_start(service_name, user, &pam_conv, &pamh);
1314 }''', dependencies: pam)
1316 if get_option('auth_pam').enabled()
1317 error('could not link libpam')
1319 warning('could not link libpam, disabling')
1324 if not get_option('snappy').auto() or have_system
1325 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'],
1326 required: get_option('snappy'),
1327 kwargs: static_kwargs)
1329 if snappy.found() and not linker.links('''
1330 #include <snappy-c.h>
1331 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy)
1333 if get_option('snappy').enabled()
1334 error('could not link libsnappy')
1336 warning('could not link libsnappy, disabling')
1341 if not get_option('lzo').auto() or have_system
1342 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'],
1343 required: get_option('lzo'),
1344 kwargs: static_kwargs)
1346 if lzo.found() and not cc.links('''
1347 #include <lzo/lzo1x.h>
1348 int main(void) { lzo_version(); return 0; }''', dependencies: lzo)
1350 if get_option('lzo').enabled()
1351 error('could not link liblzo2')
1353 warning('could not link liblzo2, disabling')
1358 if not get_option('numa').auto() or have_system or have_tools
1359 numa = cc.find_library('numa', has_headers: ['numa.h'],
1360 required: get_option('numa'),
1361 kwargs: static_kwargs)
1363 if numa.found() and not cc.links('''
1365 int main(void) { return numa_available(); }
1366 ''', dependencies: numa)
1368 if get_option('numa').enabled()
1369 error('could not link numa')
1371 warning('could not link numa, disabling')
1376 if not get_option('rdma').auto() or have_system
1377 libumad = cc.find_library('ibumad', required: get_option('rdma'))
1378 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'],
1379 required: get_option('rdma'),
1380 kwargs: static_kwargs),
1381 cc.find_library('ibverbs', required: get_option('rdma'),
1382 kwargs: static_kwargs),
1384 rdma = declare_dependency(dependencies: rdma_libs)
1385 foreach lib: rdma_libs
1393 if get_option('xen').enabled() or (get_option('xen').auto() and have_system)
1394 xencontrol = dependency('xencontrol', required: false,
1395 method: 'pkg-config', kwargs: static_kwargs)
1396 if xencontrol.found()
1397 xen_pc = declare_dependency(version: xencontrol.version(),
1400 # disabler: true makes xen_pc.found() return false if any is not found
1401 dependency('xenstore', required: false,
1402 method: 'pkg-config', kwargs: static_kwargs,
1404 dependency('xenforeignmemory', required: false,
1405 method: 'pkg-config', kwargs: static_kwargs,
1407 dependency('xengnttab', required: false,
1408 method: 'pkg-config', kwargs: static_kwargs,
1410 dependency('xenevtchn', required: false,
1411 method: 'pkg-config', kwargs: static_kwargs,
1413 dependency('xendevicemodel', required: false,
1414 method: 'pkg-config', kwargs: static_kwargs,
1416 # optional, no "disabler: true"
1417 dependency('xentoolcore', required: false,
1418 method: 'pkg-config', kwargs: static_kwargs)])
1424 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' ]
1426 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1427 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ],
1428 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1429 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1430 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ],
1431 '4.6.0': [ 'xenstore', 'xenctrl' ],
1432 '4.5.0': [ 'xenstore', 'xenctrl' ],
1433 '4.2.0': [ 'xenstore', 'xenctrl' ],
1436 foreach ver: xen_tests
1437 # cache the various library tests to avoid polluting the logs
1439 foreach l: xen_libs[ver]
1440 if l not in xen_deps
1441 xen_deps += { l: cc.find_library(l, required: false) }
1443 xen_test_deps += xen_deps[l]
1446 # Use -D to pick just one of the test programs in scripts/xen-detect.c
1447 xen_version = ver.split('.')
1448 xen_ctrl_version = xen_version[0] + \
1449 ('0' + xen_version[1]).substring(-2) + \
1450 ('0' + xen_version[2]).substring(-2)
1451 if cc.links(files('scripts/xen-detect.c'),
1452 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version,
1453 dependencies: xen_test_deps)
1454 xen = declare_dependency(version: ver, dependencies: xen_test_deps)
1460 accelerators += 'CONFIG_XEN'
1461 elif get_option('xen').enabled()
1462 error('could not compile and link Xen test program')
1465 have_xen_pci_passthrough = get_option('xen_pci_passthrough') \
1466 .require(xen.found(),
1467 error_message: 'Xen PCI passthrough requested but Xen not enabled') \
1468 .require(targetos == 'linux',
1469 error_message: 'Xen PCI passthrough not available on this platform') \
1474 if not get_option('smartcard').auto() or have_system
1475 cacard = dependency('libcacard', required: get_option('smartcard'),
1476 version: '>=2.5.1', method: 'pkg-config',
1477 kwargs: static_kwargs)
1481 u2f = dependency('u2f-emu', required: get_option('u2f'),
1482 method: 'pkg-config',
1483 kwargs: static_kwargs)
1487 canokey = dependency('canokey-qemu', required: get_option('canokey'),
1488 method: 'pkg-config',
1489 kwargs: static_kwargs)
1491 usbredir = not_found
1492 if not get_option('usb_redir').auto() or have_system
1493 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'),
1494 version: '>=0.6', method: 'pkg-config',
1495 kwargs: static_kwargs)
1498 if not get_option('libusb').auto() or have_system
1499 libusb = dependency('libusb-1.0', required: get_option('libusb'),
1500 version: '>=1.0.13', method: 'pkg-config',
1501 kwargs: static_kwargs)
1505 if not get_option('libpmem').auto() or have_system
1506 libpmem = dependency('libpmem', required: get_option('libpmem'),
1507 method: 'pkg-config', kwargs: static_kwargs)
1509 libdaxctl = not_found
1510 if not get_option('libdaxctl').auto() or have_system
1511 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'),
1512 version: '>=57', method: 'pkg-config',
1513 kwargs: static_kwargs)
1517 tasn1 = dependency('libtasn1',
1518 method: 'pkg-config',
1519 kwargs: static_kwargs)
1521 keyutils = dependency('libkeyutils', required: false,
1522 method: 'pkg-config', kwargs: static_kwargs)
1524 has_gettid = cc.has_function('gettid')
1527 selinux = dependency('libselinux',
1528 required: get_option('selinux'),
1529 method: 'pkg-config', kwargs: static_kwargs)
1534 if get_option('malloc') == 'system'
1536 get_option('malloc_trim').allowed() and \
1537 cc.links('''#include <malloc.h>
1538 int main(void) { malloc_trim(0); return 0; }''')
1540 has_malloc_trim = false
1541 malloc = cc.find_library(get_option('malloc'), required: true)
1543 if not has_malloc_trim and get_option('malloc_trim').enabled()
1544 if get_option('malloc') == 'system'
1545 error('malloc_trim not available on this platform.')
1547 error('malloc_trim not available with non-libc memory allocator')
1551 # Check whether the glibc provides statx()
1553 gnu_source_prefix = '''
1558 statx_test = gnu_source_prefix + '''
1559 #include <sys/stat.h>
1561 struct statx statxbuf;
1562 statx(0, "", 0, STATX_BASIC_STATS, &statxbuf);
1566 has_statx = cc.links(statx_test)
1568 # Check whether statx() provides mount ID information
1570 statx_mnt_id_test = gnu_source_prefix + '''
1571 #include <sys/stat.h>
1573 struct statx statxbuf;
1574 statx(0, "", 0, STATX_BASIC_STATS | STATX_MNT_ID, &statxbuf);
1575 return statxbuf.stx_mnt_id;
1578 has_statx_mnt_id = cc.links(statx_mnt_id_test)
1580 have_vhost_user_blk_server = get_option('vhost_user_blk_server') \
1581 .require(targetos == 'linux',
1582 error_message: 'vhost_user_blk_server requires linux') \
1583 .require(have_vhost_user,
1584 error_message: 'vhost_user_blk_server requires vhost-user support') \
1585 .disable_auto_if(not have_tools and not have_system) \
1588 if get_option('fuse').disabled() and get_option('fuse_lseek').enabled()
1589 error('Cannot enable fuse-lseek while fuse is disabled')
1592 fuse = dependency('fuse3', required: get_option('fuse'),
1593 version: '>=3.1', method: 'pkg-config',
1594 kwargs: static_kwargs)
1596 fuse_lseek = not_found
1597 if get_option('fuse_lseek').allowed()
1598 if fuse.version().version_compare('>=3.8')
1600 fuse_lseek = declare_dependency()
1601 elif get_option('fuse_lseek').enabled()
1603 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version())
1605 error('fuse-lseek requires libfuse, which was not found')
1610 have_libvduse = (targetos == 'linux')
1611 if get_option('libvduse').enabled()
1612 if targetos != 'linux'
1613 error('libvduse requires linux')
1615 elif get_option('libvduse').disabled()
1616 have_libvduse = false
1619 have_vduse_blk_export = (have_libvduse and targetos == 'linux')
1620 if get_option('vduse_blk_export').enabled()
1621 if targetos != 'linux'
1622 error('vduse_blk_export requires linux')
1623 elif not have_libvduse
1624 error('vduse_blk_export requires libvduse support')
1626 elif get_option('vduse_blk_export').disabled()
1627 have_vduse_blk_export = false
1631 libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config')
1632 if libbpf.found() and not cc.links('''
1633 #include <bpf/libbpf.h>
1636 bpf_object__destroy_skeleton(NULL);
1638 }''', dependencies: libbpf)
1640 if get_option('bpf').enabled()
1641 error('libbpf skeleton test failed')
1643 warning('libbpf skeleton test failed, disabling')
1649 if not get_option('libdw').auto() or \
1650 (not enable_static and (have_system or have_user))
1651 libdw = dependency('libdw',
1652 method: 'pkg-config',
1653 kwargs: static_kwargs,
1654 required: get_option('libdw'))
1661 audio_drivers_selected = []
1663 audio_drivers_available = {
1664 'alsa': alsa.found(),
1665 'coreaudio': coreaudio.found(),
1666 'dsound': dsound.found(),
1667 'jack': jack.found(),
1669 'pa': pulse.found(),
1671 'sndio': sndio.found(),
1673 foreach k, v: audio_drivers_available
1674 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v)
1677 # Default to native drivers first, OSS second, SDL third
1678 audio_drivers_priority = \
1679 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \
1680 (targetos == 'linux' ? [] : [ 'sdl' ])
1681 audio_drivers_default = []
1682 foreach k: audio_drivers_priority
1683 if audio_drivers_available[k]
1684 audio_drivers_default += k
1688 foreach k: get_option('audio_drv_list')
1690 audio_drivers_selected += audio_drivers_default
1691 elif not audio_drivers_available[k]
1692 error('Audio driver "@0@" not available.'.format(k))
1694 audio_drivers_selected += k
1698 config_host_data.set('CONFIG_AUDIO_DRIVERS',
1699 '"' + '", "'.join(audio_drivers_selected) + '", ')
1701 if get_option('cfi')
1703 # Check for dependency on LTO
1704 if not get_option('b_lto')
1705 error('Selected Control-Flow Integrity but LTO is disabled')
1707 if config_host.has_key('CONFIG_MODULES')
1708 error('Selected Control-Flow Integrity is not compatible with modules')
1710 # Check for cfi flags. CFI requires LTO so we can't use
1711 # get_supported_arguments, but need a more complex "compiles" which allows
1713 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall',
1714 args: ['-flto', '-fsanitize=cfi-icall'] )
1715 cfi_flags += '-fsanitize=cfi-icall'
1717 error('-fsanitize=cfi-icall is not supported by the compiler')
1719 if cc.compiles('int main () { return 0; }',
1720 name: '-fsanitize-cfi-icall-generalize-pointers',
1721 args: ['-flto', '-fsanitize=cfi-icall',
1722 '-fsanitize-cfi-icall-generalize-pointers'] )
1723 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers'
1725 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler')
1727 if get_option('cfi_debug')
1728 if cc.compiles('int main () { return 0; }',
1729 name: '-fno-sanitize-trap=cfi-icall',
1730 args: ['-flto', '-fsanitize=cfi-icall',
1731 '-fno-sanitize-trap=cfi-icall'] )
1732 cfi_flags += '-fno-sanitize-trap=cfi-icall'
1734 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler')
1737 add_global_arguments(cfi_flags, native: false, language: all_languages)
1738 add_global_link_arguments(cfi_flags, native: false, language: all_languages)
1741 have_host_block_device = (targetos != 'darwin' or
1742 cc.has_header('IOKit/storage/IOMedia.h'))
1744 dbus_display = get_option('dbus_display') \
1745 .require(gio.version().version_compare('>=2.64'),
1746 error_message: '-display dbus requires glib>=2.64') \
1747 .require(gdbus_codegen.found(),
1748 error_message: gdbus_codegen_error.format('-display dbus')) \
1749 .require(opengl.found() and gbm.found(),
1750 error_message: '-display dbus requires epoxy/egl and gbm') \
1753 have_virtfs = get_option('virtfs') \
1754 .require(targetos == 'linux' or targetos == 'darwin',
1755 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \
1756 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'),
1757 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \
1758 .require(targetos == 'darwin' or (libattr.found() and libcap_ng.found()),
1759 error_message: 'virtio-9p (virtfs) on Linux requires libcap-ng-devel and libattr-devel') \
1760 .disable_auto_if(not have_tools and not have_system) \
1763 have_virtfs_proxy_helper = targetos != 'darwin' and have_virtfs and have_tools
1765 if get_option('block_drv_ro_whitelist') == ''
1766 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '')
1768 config_host_data.set('CONFIG_BDRV_RO_WHITELIST',
1769 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ')
1771 if get_option('block_drv_rw_whitelist') == ''
1772 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '')
1774 config_host_data.set('CONFIG_BDRV_RW_WHITELIST',
1775 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ')
1778 foreach k : get_option('trace_backends')
1779 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true)
1781 config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file'))
1782 config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority'))
1784 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path())
1786 config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir'))
1787 config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix'))
1788 config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir)
1789 config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir)
1790 config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir)
1792 qemu_firmwarepath = ''
1793 foreach k : get_option('qemu_firmwarepath')
1794 qemu_firmwarepath += '"' + get_option('prefix') / k + '", '
1796 config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath)
1798 config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir'))
1799 config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir)
1800 config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir'))
1801 config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir'))
1802 config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir)
1803 config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir'))
1805 if config_host.has_key('CONFIG_MODULES')
1806 config_host_data.set('CONFIG_STAMP', run_command(
1807 meson.current_source_dir() / 'scripts/qemu-stamp.py',
1808 meson.project_version(), get_option('pkgversion'), '--',
1809 meson.current_source_dir() / 'configure',
1810 capture: true, check: true).stdout().strip())
1813 have_slirp_smbd = get_option('slirp_smbd') \
1814 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \
1817 smbd_path = get_option('smbd')
1819 smbd_path = (targetos == 'solaris' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd')
1821 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path)
1824 config_host_data.set('HOST_' + host_arch.to_upper(), 1)
1826 if get_option('module_upgrades') and not enable_modules
1827 error('Cannot enable module-upgrades as modules are not enabled')
1829 config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades'))
1831 config_host_data.set('CONFIG_ATTR', libattr.found())
1832 config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools'))
1833 config_host_data.set('CONFIG_BRLAPI', brlapi.found())
1834 config_host_data.set('CONFIG_COCOA', cocoa.found())
1835 config_host_data.set('CONFIG_FUZZ', get_option('fuzzing'))
1836 config_host_data.set('CONFIG_GCOV', get_option('b_coverage'))
1837 config_host_data.set('CONFIG_LIBUDEV', libudev.found())
1838 config_host_data.set('CONFIG_LZO', lzo.found())
1839 config_host_data.set('CONFIG_MPATH', mpathpersist.found())
1840 config_host_data.set('CONFIG_MPATH_NEW_API', mpathpersist_new_api)
1841 config_host_data.set('CONFIG_BLKIO', blkio.found())
1842 config_host_data.set('CONFIG_CURL', curl.found())
1843 config_host_data.set('CONFIG_CURSES', curses.found())
1844 config_host_data.set('CONFIG_GBM', gbm.found())
1845 config_host_data.set('CONFIG_GIO', gio.found())
1846 config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found())
1847 if glusterfs.found()
1848 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4'))
1849 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5'))
1850 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6'))
1851 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6'))
1852 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat)
1853 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat)
1855 config_host_data.set('CONFIG_GTK', gtk.found())
1856 config_host_data.set('CONFIG_VTE', vte.found())
1857 config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard)
1858 config_host_data.set('CONFIG_LIBATTR', have_old_libattr)
1859 config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found())
1860 config_host_data.set('CONFIG_EBPF', libbpf.found())
1861 config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found())
1862 config_host_data.set('CONFIG_LIBISCSI', libiscsi.found())
1863 config_host_data.set('CONFIG_LIBNFS', libnfs.found())
1864 config_host_data.set('CONFIG_LIBSSH', libssh.found())
1865 config_host_data.set('CONFIG_LINUX_AIO', libaio.found())
1866 config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found())
1867 config_host_data.set('CONFIG_LIBPMEM', libpmem.found())
1868 config_host_data.set('CONFIG_NUMA', numa.found())
1870 config_host_data.set('HAVE_NUMA_HAS_PREFERRED_MANY',
1871 cc.has_function('numa_has_preferred_many',
1872 dependencies: numa))
1874 config_host_data.set('CONFIG_OPENGL', opengl.found())
1875 config_host_data.set('CONFIG_PROFILER', get_option('profiler'))
1876 config_host_data.set('CONFIG_RBD', rbd.found())
1877 config_host_data.set('CONFIG_RDMA', rdma.found())
1878 config_host_data.set('CONFIG_SDL', sdl.found())
1879 config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found())
1880 config_host_data.set('CONFIG_SECCOMP', seccomp.found())
1882 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc)
1884 config_host_data.set('CONFIG_SNAPPY', snappy.found())
1885 config_host_data.set('CONFIG_TPM', have_tpm)
1886 config_host_data.set('CONFIG_USB_LIBUSB', libusb.found())
1887 config_host_data.set('CONFIG_VDE', vde.found())
1888 config_host_data.set('CONFIG_VHOST_NET', have_vhost_net)
1889 config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user)
1890 config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa)
1891 config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel)
1892 config_host_data.set('CONFIG_VHOST_USER', have_vhost_user)
1893 config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto)
1894 config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa)
1895 config_host_data.set('CONFIG_VMNET', vmnet.found())
1896 config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server)
1897 config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export)
1898 config_host_data.set('CONFIG_PNG', png.found())
1899 config_host_data.set('CONFIG_VNC', vnc.found())
1900 config_host_data.set('CONFIG_VNC_JPEG', jpeg.found())
1901 config_host_data.set('CONFIG_VNC_SASL', sasl.found())
1902 config_host_data.set('CONFIG_VIRTFS', have_virtfs)
1903 config_host_data.set('CONFIG_VTE', vte.found())
1904 config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found())
1905 config_host_data.set('CONFIG_KEYUTILS', keyutils.found())
1906 config_host_data.set('CONFIG_GETTID', has_gettid)
1907 config_host_data.set('CONFIG_GNUTLS', gnutls.found())
1908 config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found())
1909 config_host_data.set('CONFIG_TASN1', tasn1.found())
1910 config_host_data.set('CONFIG_GCRYPT', gcrypt.found())
1911 config_host_data.set('CONFIG_NETTLE', nettle.found())
1912 config_host_data.set('CONFIG_HOGWEED', hogweed.found())
1913 config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private')
1914 config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim)
1915 config_host_data.set('CONFIG_STATX', has_statx)
1916 config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id)
1917 config_host_data.set('CONFIG_ZSTD', zstd.found())
1918 config_host_data.set('CONFIG_FUSE', fuse.found())
1919 config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found())
1920 config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found())
1921 if spice_protocol.found()
1922 config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0])
1923 config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1])
1924 config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2])
1926 config_host_data.set('CONFIG_SPICE', spice.found())
1927 config_host_data.set('CONFIG_X11', x11.found())
1928 config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display)
1929 config_host_data.set('CONFIG_CFI', get_option('cfi'))
1930 config_host_data.set('CONFIG_SELINUX', selinux.found())
1931 config_host_data.set('CONFIG_XEN_BACKEND', xen.found())
1932 config_host_data.set('CONFIG_LIBDW', libdw.found())
1934 # protect from xen.version() having less than three components
1935 xen_version = xen.version().split('.') + ['0', '0']
1936 xen_ctrl_version = xen_version[0] + \
1937 ('0' + xen_version[1]).substring(-2) + \
1938 ('0' + xen_version[2]).substring(-2)
1939 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version)
1941 config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version()))
1942 config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0])
1943 config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1])
1944 config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2])
1946 config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf)
1947 config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device)
1949 have_coroutine_pool = get_option('coroutine_pool')
1950 if get_option('debug_stack_usage') and have_coroutine_pool
1951 message('Disabling coroutine pool to measure stack usage')
1952 have_coroutine_pool = false
1954 config_host_data.set10('CONFIG_COROUTINE_POOL', have_coroutine_pool)
1955 config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex'))
1956 config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage'))
1957 config_host_data.set('CONFIG_GPROF', get_option('gprof'))
1958 config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed())
1959 config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug'))
1960 config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed())
1963 config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h'))
1964 config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h'))
1965 config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h'))
1966 config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h'))
1967 config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h'))
1968 config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h'))
1969 config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h'))
1970 config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h'))
1971 config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h'))
1972 if targetos == 'windows'
1973 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h'))
1977 config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range'))
1978 config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4'))
1979 config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime'))
1980 config_host_data.set('CONFIG_DUP3', cc.has_function('dup3'))
1981 config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate'))
1982 config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate'))
1983 # Note that we need to specify prefix: here to avoid incorrectly
1984 # thinking that Windows has posix_memalign()
1985 config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>'))
1986 config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc'))
1987 config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc'))
1988 config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign'))
1989 config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll'))
1990 config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>'))
1991 config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np'))
1992 config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile'))
1993 config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare'))
1994 config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs'))
1995 config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range'))
1996 config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create'))
1997 config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range'))
1998 config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs'))
1999 config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util))
2000 config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul'))
2001 config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>'))
2003 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS',
2004 cc.has_function('rbd_namespace_exists',
2006 prefix: '#include <rbd/librbd.h>'))
2009 config_host_data.set('HAVE_IBV_ADVISE_MR',
2010 cc.has_function('ibv_advise_mr',
2012 prefix: '#include <infiniband/verbs.h>'))
2016 config_host_data.set('CONFIG_EPOLL_CREATE1',
2017 cc.has_header_symbol('sys/epoll.h', 'epoll_create1'))
2018 config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE',
2019 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and
2020 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE'))
2021 config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE',
2022 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE'))
2023 config_host_data.set('CONFIG_FIEMAP',
2024 cc.has_header('linux/fiemap.h') and
2025 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP'))
2026 config_host_data.set('CONFIG_GETRANDOM',
2027 cc.has_function('getrandom') and
2028 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK'))
2029 config_host_data.set('CONFIG_INOTIFY',
2030 cc.has_header_symbol('sys/inotify.h', 'inotify_init'))
2031 config_host_data.set('CONFIG_INOTIFY1',
2032 cc.has_header_symbol('sys/inotify.h', 'inotify_init1'))
2033 config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK',
2034 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK'))
2035 config_host_data.set('CONFIG_RTNETLINK',
2036 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN'))
2037 config_host_data.set('CONFIG_SYSMACROS',
2038 cc.has_header_symbol('sys/sysmacros.h', 'makedev'))
2039 config_host_data.set('HAVE_OPTRESET',
2040 cc.has_header_symbol('getopt.h', 'optreset'))
2041 config_host_data.set('HAVE_IPPROTO_MPTCP',
2042 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP'))
2045 config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID',
2046 cc.has_member('struct sigevent', 'sigev_notify_thread_id',
2047 prefix: '#include <signal.h>'))
2048 config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM',
2049 cc.has_member('struct stat', 'st_atim',
2050 prefix: '#include <sys/stat.h>'))
2053 config_host_data.set('CONFIG_IOVEC',
2054 cc.has_type('struct iovec',
2055 prefix: '#include <sys/uio.h>'))
2056 config_host_data.set('HAVE_UTMPX',
2057 cc.has_type('struct utmpx',
2058 prefix: '#include <utmpx.h>'))
2060 config_host_data.set('CONFIG_EVENTFD', cc.links('''
2061 #include <sys/eventfd.h>
2062 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }'''))
2063 config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + '''
2066 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
2067 return fdatasync(0);
2069 #error Not supported
2073 has_madvise = cc.links(gnu_source_prefix + '''
2074 #include <sys/types.h>
2075 #include <sys/mman.h>
2077 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''')
2078 missing_madvise_proto = false
2080 # Some platforms (illumos and Solaris before Solaris 11) provide madvise()
2081 # but forget to prototype it. In this case, has_madvise will be true (the
2082 # test program links despite a compile warning). To detect the
2083 # missing-prototype case, we try again with a definitely-bogus prototype.
2084 # This will only compile if the system headers don't provide the prototype;
2085 # otherwise the conflicting prototypes will cause a compiler error.
2086 missing_madvise_proto = cc.links(gnu_source_prefix + '''
2087 #include <sys/types.h>
2088 #include <sys/mman.h>
2090 extern int madvise(int);
2091 int main(void) { return madvise(0); }''')
2093 config_host_data.set('CONFIG_MADVISE', has_madvise)
2094 config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto)
2096 config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + '''
2097 #include <sys/mman.h>
2098 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }'''))
2099 config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + '''
2101 #if !defined(AT_EMPTY_PATH)
2102 # error missing definition
2104 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
2106 config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + '''
2107 #include <sys/mman.h>
2109 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }'''))
2111 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + '''
2112 #include <pthread.h>
2114 static void *f(void *p) { return NULL; }
2118 pthread_create(&thread, 0, f, 0);
2119 pthread_setname_np(thread, "QEMU");
2121 }''', dependencies: threads))
2122 config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + '''
2123 #include <pthread.h>
2125 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
2129 pthread_create(&thread, 0, f, 0);
2131 }''', dependencies: threads))
2132 config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + '''
2133 #include <pthread.h>
2138 pthread_condattr_t attr
2139 pthread_condattr_init(&attr);
2140 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC);
2142 }''', dependencies: threads))
2143 config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + '''
2144 #include <pthread.h>
2146 static void *f(void *p) { return NULL; }
2149 int setsize = CPU_ALLOC_SIZE(64);
2152 pthread_create(&thread, 0, f, 0);
2153 cpuset = CPU_ALLOC(64);
2154 CPU_ZERO_S(setsize, cpuset);
2155 pthread_setaffinity_np(thread, setsize, cpuset);
2156 pthread_getaffinity_np(thread, setsize, cpuset);
2159 }''', dependencies: threads))
2160 config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + '''
2161 #include <sys/signalfd.h>
2163 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }'''))
2164 config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + '''
2172 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
2173 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
2177 config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + '''
2178 #include <sys/mman.h>
2180 return mlockall(MCL_FUTURE);
2184 if get_option('l2tpv3').allowed() and have_system
2185 have_l2tpv3 = cc.has_type('struct mmsghdr',
2186 prefix: gnu_source_prefix + '''
2187 #include <sys/socket.h>
2188 #include <linux/ip.h>''')
2190 config_host_data.set('CONFIG_L2TPV3', have_l2tpv3)
2193 if get_option('netmap').allowed() and have_system
2194 have_netmap = cc.compiles('''
2195 #include <inttypes.h>
2197 #include <net/netmap.h>
2198 #include <net/netmap_user.h>
2199 #if (NETMAP_API < 11) || (NETMAP_API > 15)
2202 int main(void) { return 0; }''')
2203 if not have_netmap and get_option('netmap').enabled()
2204 error('Netmap headers not available')
2207 config_host_data.set('CONFIG_NETMAP', have_netmap)
2209 # Work around a system header bug with some kernel/XFS header
2210 # versions where they both try to define 'struct fsxattr':
2211 # xfs headers will not try to redefine structs from linux headers
2212 # if this macro is set.
2213 config_host_data.set('HAVE_FSXATTR', cc.links('''
2214 #include <linux/fs.h>
2220 # Some versions of Mac OS X incorrectly define SIZE_MAX
2221 config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles('''
2225 return printf("%zu", SIZE_MAX);
2226 }''', args: ['-Werror']))
2233 y = __atomic_load_n(&x, __ATOMIC_RELAXED);
2234 __atomic_store_n(&x, y, __ATOMIC_RELAXED);
2235 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
2236 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
2237 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
2241 # See if 64-bit atomic operations are supported.
2242 # Note that without __atomic builtins, we can only
2243 # assume atomic loads/stores max at pointer size.
2244 config_host_data.set('CONFIG_ATOMIC64', cc.links(atomic_test.format('uint64_t')))
2246 has_int128 = cc.links('''
2256 config_host_data.set('CONFIG_INT128', has_int128)
2259 # "do we have 128-bit atomics which are handled inline and specifically not
2260 # via libatomic". The reason we can't use libatomic is documented in the
2261 # comment starting "GCC is a house divided" in include/qemu/atomic128.h.
2262 has_atomic128 = cc.links(atomic_test.format('unsigned __int128'))
2264 config_host_data.set('CONFIG_ATOMIC128', has_atomic128)
2266 if not has_atomic128
2267 has_cmpxchg128 = cc.links('''
2270 unsigned __int128 x = 0, y = 0;
2271 __sync_val_compare_and_swap_16(&x, y, x);
2276 config_host_data.set('CONFIG_CMPXCHG128', has_cmpxchg128)
2280 config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + '''
2281 #include <sys/auxv.h>
2283 return getauxval(AT_HWCAP) == 0;
2286 config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles('''
2287 #include <linux/usbdevice_fs.h>
2289 #ifndef USBDEVFS_GET_CAPABILITIES
2290 #error "USBDEVFS_GET_CAPABILITIES undefined"
2293 #ifndef USBDEVFS_DISCONNECT_CLAIM
2294 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
2297 int main(void) { return 0; }'''))
2299 have_keyring = get_option('keyring') \
2300 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \
2301 .require(cc.compiles('''
2303 #include <asm/unistd.h>
2304 #include <linux/keyctl.h>
2305 #include <sys/syscall.h>
2308 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
2309 }'''), error_message: 'keyctl syscall not available on this system').allowed()
2310 config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring)
2312 have_cpuid_h = cc.links('''
2315 unsigned a, b, c, d;
2316 unsigned max = __get_cpuid_max(0, 0);
2319 __cpuid(1, a, b, c, d);
2323 __cpuid_count(7, 0, a, b, c, d);
2328 config_host_data.set('CONFIG_CPUID_H', have_cpuid_h)
2330 config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \
2331 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \
2332 .require(cc.links('''
2334 #include <immintrin.h>
2335 static int __attribute__((target("avx2"))) bar(void *a) {
2336 __m256i x = *(__m256i *)a;
2337 return _mm256_testz_si256(x, x);
2339 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2340 '''), error_message: 'AVX2 not available').allowed())
2342 config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \
2343 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \
2344 .require(cc.links('''
2346 #include <immintrin.h>
2347 static int __attribute__((target("avx512f"))) bar(void *a) {
2348 __m512i x = *(__m512i *)a;
2349 return _mm512_test_epi64_mask(x, x);
2351 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); }
2352 '''), error_message: 'AVX512F not available').allowed())
2354 config_host_data.set('CONFIG_AVX512BW_OPT', get_option('avx512bw') \
2355 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512BW') \
2356 .require(cc.links('''
2357 #pragma GCC push_options
2358 #pragma GCC target("avx512bw")
2360 #include <immintrin.h>
2361 static int bar(void *a) {
2364 __m512i res= _mm512_abs_epi8(*x);
2367 int main(int argc, char *argv[]) { return bar(argv[0]); }
2368 '''), error_message: 'AVX512BW not available').allowed())
2370 have_pvrdma = get_option('pvrdma') \
2371 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \
2372 .require(cc.compiles(gnu_source_prefix + '''
2373 #include <sys/mman.h>
2378 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
2381 }'''), error_message: 'PVRDMA requires mremap').allowed()
2384 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links('''
2385 #include <infiniband/verbs.h>
2389 struct ibv_pd *pd = NULL;
2395 mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
2401 if get_option('membarrier').disabled()
2402 have_membarrier = false
2403 elif targetos == 'windows'
2404 have_membarrier = true
2405 elif targetos == 'linux'
2406 have_membarrier = cc.compiles('''
2407 #include <linux/membarrier.h>
2408 #include <sys/syscall.h>
2412 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
2413 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
2417 config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \
2418 .require(have_membarrier, error_message: 'membarrier system call not available') \
2421 have_afalg = get_option('crypto_afalg') \
2422 .require(cc.compiles(gnu_source_prefix + '''
2424 #include <sys/types.h>
2425 #include <sys/socket.h>
2426 #include <linux/if_alg.h>
2429 sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
2432 '''), error_message: 'AF_ALG requested but could not be detected').allowed()
2433 config_host_data.set('CONFIG_AF_ALG', have_afalg)
2435 config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol(
2436 'linux/vm_sockets.h', 'AF_VSOCK',
2437 prefix: '#include <sys/socket.h>',
2441 have_vss_sdk = false # old xp/2003 SDK
2442 if targetos == 'windows' and link_language == 'cpp'
2443 have_vss = cxx.compiles('''
2444 #define __MIDL_user_allocate_free_DEFINED__
2446 int main(void) { return VSS_CTX_BACKUP; }''')
2447 have_vss_sdk = cxx.has_header('vscoordint.h')
2449 config_host_data.set('HAVE_VSS_SDK', have_vss_sdk)
2451 foreach k, v: config_host
2452 if k.startswith('CONFIG_')
2453 config_host_data.set(k, v == 'y' ? 1 : v)
2457 # Older versions of MinGW do not import _lock_file and _unlock_file properly.
2458 # This was fixed for v6.0.0 with commit b48e3ac8969d.
2459 if targetos == 'windows'
2460 config_host_data.set('HAVE__LOCK_FILE', cc.links('''
2466 }''', name: '_lock_file and _unlock_file'))
2469 ########################
2470 # Target configuration #
2471 ########################
2473 minikconf = find_program('scripts/minikconf.py')
2475 config_all_devices = {}
2476 config_all_disas = {}
2477 config_devices_mak_list = []
2478 config_devices_h = {}
2479 config_target_h = {}
2480 config_target_mak = {}
2483 'alpha' : ['CONFIG_ALPHA_DIS'],
2484 'avr' : ['CONFIG_AVR_DIS'],
2485 'cris' : ['CONFIG_CRIS_DIS'],
2486 'hexagon' : ['CONFIG_HEXAGON_DIS'],
2487 'hppa' : ['CONFIG_HPPA_DIS'],
2488 'i386' : ['CONFIG_I386_DIS'],
2489 'x86_64' : ['CONFIG_I386_DIS'],
2490 'm68k' : ['CONFIG_M68K_DIS'],
2491 'microblaze' : ['CONFIG_MICROBLAZE_DIS'],
2492 'mips' : ['CONFIG_MIPS_DIS'],
2493 'nios2' : ['CONFIG_NIOS2_DIS'],
2494 'or1k' : ['CONFIG_OPENRISC_DIS'],
2495 'ppc' : ['CONFIG_PPC_DIS'],
2496 'riscv' : ['CONFIG_RISCV_DIS'],
2497 'rx' : ['CONFIG_RX_DIS'],
2498 's390' : ['CONFIG_S390_DIS'],
2499 'sh4' : ['CONFIG_SH4_DIS'],
2500 'sparc' : ['CONFIG_SPARC_DIS'],
2501 'xtensa' : ['CONFIG_XTENSA_DIS'],
2502 'loongarch' : ['CONFIG_LOONGARCH_DIS'],
2505 have_ivshmem = config_host_data.get('CONFIG_EVENTFD')
2507 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \
2508 (have_tpm ? ['CONFIG_TPM=y'] : []) + \
2509 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \
2510 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \
2511 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \
2512 (x11.found() ? ['CONFIG_X11=y'] : []) + \
2513 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \
2514 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \
2515 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \
2516 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \
2517 ('CONFIG_LINUX' in config_host ? ['CONFIG_LINUX=y'] : []) + \
2518 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \
2519 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \
2520 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : [])
2522 ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ]
2524 default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host
2525 actual_target_dirs = []
2527 foreach target : target_dirs
2528 config_target = { 'TARGET_NAME': target.split('-')[0] }
2529 if target.endswith('linux-user')
2530 if targetos != 'linux'
2534 error('Target @0@ is only available on a Linux host'.format(target))
2536 config_target += { 'CONFIG_LINUX_USER': 'y' }
2537 elif target.endswith('bsd-user')
2538 if 'CONFIG_BSD' not in config_host
2542 error('Target @0@ is only available on a BSD host'.format(target))
2544 config_target += { 'CONFIG_BSD_USER': 'y' }
2545 elif target.endswith('softmmu')
2546 config_target += { 'CONFIG_SOFTMMU': 'y' }
2548 if target.endswith('-user')
2550 'CONFIG_USER_ONLY': 'y',
2551 'CONFIG_QEMU_INTERP_PREFIX':
2552 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME'])
2557 foreach sym: accelerators
2558 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, [])
2559 config_target += { sym: 'y' }
2560 config_all += { sym: 'y' }
2561 if target in modular_tcg
2562 config_target += { 'CONFIG_TCG_MODULAR': 'y' }
2564 config_target += { 'CONFIG_TCG_BUILTIN': 'y' }
2566 accel_kconfig += [ sym + '=y' ]
2569 if accel_kconfig.length() == 0
2573 error('No accelerator available for target @0@'.format(target))
2576 actual_target_dirs += target
2577 config_target += keyval.load('configs/targets' / target + '.mak')
2578 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' }
2580 if 'TARGET_NEED_FDT' in config_target
2581 fdt_required += target
2585 if 'TARGET_BASE_ARCH' not in config_target
2586 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']}
2588 if 'TARGET_ABI_DIR' not in config_target
2589 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']}
2591 if 'TARGET_BIG_ENDIAN' not in config_target
2592 config_target += {'TARGET_BIG_ENDIAN': 'n'}
2595 foreach k, v: disassemblers
2596 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k)
2598 config_target += { sym: 'y' }
2599 config_all_disas += { sym: 'y' }
2604 config_target_data = configuration_data()
2605 foreach k, v: config_target
2606 if not k.startswith('TARGET_') and not k.startswith('CONFIG_')
2608 elif ignored.contains(k)
2610 elif k == 'TARGET_BASE_ARCH'
2611 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is
2612 # not used to select files from sourcesets.
2613 config_target_data.set('TARGET_' + v.to_upper(), 1)
2614 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX'
2615 config_target_data.set_quoted(k, v)
2617 config_target_data.set(k, 1)
2619 config_target_data.set(k, 0)
2621 config_target_data.set(k, v)
2624 config_target_data.set('QEMU_ARCH',
2625 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper())
2626 config_target_h += {target: configure_file(output: target + '-config-target.h',
2627 configuration: config_target_data)}
2629 if target.endswith('-softmmu')
2630 config_input = meson.get_external_property(target, 'default')
2631 config_devices_mak = target + '-config-devices.mak'
2632 config_devices_mak = configure_file(
2633 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'],
2634 output: config_devices_mak,
2635 depfile: config_devices_mak + '.d',
2637 command: [minikconf,
2638 get_option('default_devices') ? '--defconfig' : '--allnoconfig',
2639 config_devices_mak, '@DEPFILE@', '@INPUT@',
2640 host_kconfig, accel_kconfig,
2641 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y'])
2643 config_devices_data = configuration_data()
2644 config_devices = keyval.load(config_devices_mak)
2645 foreach k, v: config_devices
2646 config_devices_data.set(k, 1)
2648 config_devices_mak_list += config_devices_mak
2649 config_devices_h += {target: configure_file(output: target + '-config-devices.h',
2650 configuration: config_devices_data)}
2651 config_target += config_devices
2652 config_all_devices += config_devices
2654 config_target_mak += {target: config_target}
2656 target_dirs = actual_target_dirs
2658 # This configuration is used to build files that are shared by
2659 # multiple binaries, and then extracted out of the "common"
2660 # static_library target.
2662 # We do not use all_sources()/all_dependencies(), because it would
2663 # build literally all source files, including devices only used by
2664 # targets that are not built for this compilation. The CONFIG_ALL
2665 # pseudo symbol replaces it.
2667 config_all += config_all_devices
2668 config_all += config_host
2669 config_all += config_all_disas
2671 'CONFIG_XEN': xen.found(),
2672 'CONFIG_SOFTMMU': have_system,
2673 'CONFIG_USER_ONLY': have_user,
2677 target_configs_h = []
2678 foreach target: target_dirs
2679 target_configs_h += config_target_h[target]
2680 target_configs_h += config_devices_h.get(target, [])
2682 genh += custom_target('config-poison.h',
2683 input: [target_configs_h],
2684 output: 'config-poison.h',
2686 command: [find_program('scripts/make-config-poison.sh'),
2693 capstone = not_found
2694 if not get_option('capstone').auto() or have_system or have_user
2695 capstone = dependency('capstone', version: '>=3.0.5',
2696 kwargs: static_kwargs, method: 'pkg-config',
2697 required: get_option('capstone'))
2699 # Some versions of capstone have broken pkg-config file
2700 # that reports a wrong -I path, causing the #include to
2701 # fail later. If the system has such a broken version
2703 if capstone.found() and not cc.compiles('#include <capstone.h>',
2704 dependencies: [capstone])
2705 capstone = not_found
2706 if get_option('capstone').enabled()
2707 error('capstone requested, but it does not appear to work')
2712 libvfio_user_dep = not_found
2713 if have_system and vfio_user_server_allowed
2714 have_internal = fs.exists(meson.current_source_dir() / 'subprojects/libvfio-user/meson.build')
2716 if not have_internal
2717 error('libvfio-user source not found - please pull git submodule')
2720 libvfio_user_proj = subproject('libvfio-user')
2722 libvfio_user_lib = libvfio_user_proj.get_variable('libvfio_user_dep')
2724 libvfio_user_dep = declare_dependency(dependencies: [libvfio_user_lib])
2729 fdt_opt = get_option('fdt')
2730 if fdt_opt in ['enabled', 'auto', 'system']
2731 have_internal = fs.exists(meson.current_source_dir() / 'dtc/libfdt/Makefile.libfdt')
2732 fdt = cc.find_library('fdt', kwargs: static_kwargs,
2733 required: fdt_opt == 'system' or
2734 fdt_opt == 'enabled' and not have_internal)
2735 if fdt.found() and cc.links('''
2737 #include <libfdt_env.h>
2738 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''',
2741 elif fdt_opt == 'system'
2742 error('system libfdt requested, but it is too old (1.5.1 or newer required)')
2744 fdt_opt = 'internal'
2746 fdt_opt = 'disabled'
2750 if fdt_opt == 'internal'
2753 'dtc/libfdt/fdt_ro.c',
2754 'dtc/libfdt/fdt_wip.c',
2755 'dtc/libfdt/fdt_sw.c',
2756 'dtc/libfdt/fdt_rw.c',
2757 'dtc/libfdt/fdt_strerror.c',
2758 'dtc/libfdt/fdt_empty_tree.c',
2759 'dtc/libfdt/fdt_addresses.c',
2760 'dtc/libfdt/fdt_overlay.c',
2761 'dtc/libfdt/fdt_check.c',
2764 fdt_inc = include_directories('dtc/libfdt')
2765 libfdt = static_library('fdt',
2766 build_by_default: false,
2768 include_directories: fdt_inc)
2769 fdt = declare_dependency(link_with: libfdt,
2770 include_directories: fdt_inc)
2773 fdt_opt = 'disabled'
2775 if not fdt.found() and fdt_required.length() > 0
2776 error('fdt not available but required by targets ' + ', '.join(fdt_required))
2779 config_host_data.set('CONFIG_CAPSTONE', capstone.found())
2780 config_host_data.set('CONFIG_FDT', fdt.found())
2781 config_host_data.set('CONFIG_SLIRP', slirp.found())
2783 #####################
2784 # Generated sources #
2785 #####################
2787 genh += configure_file(output: 'config-host.h', configuration: config_host_data)
2789 hxtool = find_program('scripts/hxtool')
2790 shaderinclude = find_program('scripts/shaderinclude.py')
2791 qapi_gen = find_program('scripts/qapi-gen.py')
2792 qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py',
2793 meson.current_source_dir() / 'scripts/qapi/commands.py',
2794 meson.current_source_dir() / 'scripts/qapi/common.py',
2795 meson.current_source_dir() / 'scripts/qapi/error.py',
2796 meson.current_source_dir() / 'scripts/qapi/events.py',
2797 meson.current_source_dir() / 'scripts/qapi/expr.py',
2798 meson.current_source_dir() / 'scripts/qapi/gen.py',
2799 meson.current_source_dir() / 'scripts/qapi/introspect.py',
2800 meson.current_source_dir() / 'scripts/qapi/parser.py',
2801 meson.current_source_dir() / 'scripts/qapi/schema.py',
2802 meson.current_source_dir() / 'scripts/qapi/source.py',
2803 meson.current_source_dir() / 'scripts/qapi/types.py',
2804 meson.current_source_dir() / 'scripts/qapi/visit.py',
2805 meson.current_source_dir() / 'scripts/qapi/common.py',
2806 meson.current_source_dir() / 'scripts/qapi-gen.py'
2810 python, files('scripts/tracetool.py'),
2811 '--backend=' + ','.join(get_option('trace_backends'))
2813 tracetool_depends = files(
2814 'scripts/tracetool/backend/log.py',
2815 'scripts/tracetool/backend/__init__.py',
2816 'scripts/tracetool/backend/dtrace.py',
2817 'scripts/tracetool/backend/ftrace.py',
2818 'scripts/tracetool/backend/simple.py',
2819 'scripts/tracetool/backend/syslog.py',
2820 'scripts/tracetool/backend/ust.py',
2821 'scripts/tracetool/format/ust_events_c.py',
2822 'scripts/tracetool/format/ust_events_h.py',
2823 'scripts/tracetool/format/__init__.py',
2824 'scripts/tracetool/format/d.py',
2825 'scripts/tracetool/format/simpletrace_stap.py',
2826 'scripts/tracetool/format/c.py',
2827 'scripts/tracetool/format/h.py',
2828 'scripts/tracetool/format/log_stap.py',
2829 'scripts/tracetool/format/stap.py',
2830 'scripts/tracetool/__init__.py',
2831 'scripts/tracetool/transform.py',
2832 'scripts/tracetool/vcpu.py'
2835 qemu_version_cmd = [find_program('scripts/qemu-version.sh'),
2836 meson.current_source_dir(),
2837 get_option('pkgversion'), meson.project_version()]
2838 qemu_version = custom_target('qemu-version.h',
2839 output: 'qemu-version.h',
2840 command: qemu_version_cmd,
2842 build_by_default: true,
2843 build_always_stale: true)
2844 genh += qemu_version
2848 ['qemu-options.hx', 'qemu-options.def'],
2849 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'],
2853 ['hmp-commands.hx', 'hmp-commands.h'],
2854 ['hmp-commands-info.hx', 'hmp-commands-info.h'],
2857 foreach d : hx_headers
2858 hxdep += custom_target(d[1],
2862 build_by_default: true, # to be removed when added to a target
2863 command: [hxtool, '-h', '@INPUT0@'])
2871 authz_ss = ss.source_set()
2872 blockdev_ss = ss.source_set()
2873 block_ss = ss.source_set()
2874 chardev_ss = ss.source_set()
2875 common_ss = ss.source_set()
2876 crypto_ss = ss.source_set()
2877 hwcore_ss = ss.source_set()
2878 io_ss = ss.source_set()
2879 qmp_ss = ss.source_set()
2880 qom_ss = ss.source_set()
2881 softmmu_ss = ss.source_set()
2882 specific_fuzz_ss = ss.source_set()
2883 specific_ss = ss.source_set()
2884 stub_ss = ss.source_set()
2885 trace_ss = ss.source_set()
2886 user_ss = ss.source_set()
2887 util_ss = ss.source_set()
2890 qtest_module_ss = ss.source_set()
2891 tcg_module_ss = ss.source_set()
2897 target_softmmu_arch = {}
2898 target_user_arch = {}
2904 # TODO: add each directory to the subdirs from its own meson.build, once
2906 trace_events_subdirs = [
2915 trace_events_subdirs += [ 'linux-user' ]
2918 trace_events_subdirs += [ 'bsd-user' ]
2921 trace_events_subdirs += [
2930 trace_events_subdirs += [
2944 'hw/block/dataplane',
2993 if have_system or have_user
2994 trace_events_subdirs += [
3012 vhost_user = not_found
3013 if targetos == 'linux' and have_vhost_user
3014 libvhost_user = subproject('libvhost-user')
3015 vhost_user = libvhost_user.get_variable('vhost_user_dep')
3018 libvduse = not_found
3020 libvduse_proj = subproject('libvduse')
3021 libvduse = libvduse_proj.get_variable('libvduse_dep')
3024 # NOTE: the trace/ subdirectory needs the qapi_trace_events variable
3025 # that is filled in by qapi/.
3040 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO')
3041 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO')
3044 qom_ss = qom_ss.apply(config_host, strict: false)
3045 libqom = static_library('qom', qom_ss.sources() + genh,
3046 dependencies: [qom_ss.dependencies()],
3048 qom = declare_dependency(link_whole: libqom)
3050 event_loop_base = files('event-loop-base.c')
3051 event_loop_base = static_library('event-loop-base', sources: event_loop_base + genh,
3052 build_by_default: true)
3053 event_loop_base = declare_dependency(link_whole: event_loop_base,
3054 dependencies: [qom])
3056 stub_ss = stub_ss.apply(config_all, strict: false)
3058 util_ss.add_all(trace_ss)
3059 util_ss = util_ss.apply(config_all, strict: false)
3060 libqemuutil = static_library('qemuutil',
3061 sources: util_ss.sources() + stub_ss.sources() + genh,
3062 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman])
3063 qemuutil = declare_dependency(link_with: libqemuutil,
3064 sources: genh + version_res,
3065 dependencies: [event_loop_base])
3067 if have_system or have_user
3068 decodetree = generator(find_program('scripts/decodetree.py'),
3069 output: 'decode-@BASENAME@.c.inc',
3070 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@'])
3071 subdir('libdecnumber')
3088 if config_host_data.get('CONFIG_REPLICATION')
3089 block_ss.add(files('replication.c'))
3096 blockdev_ss.add(files(
3103 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon,
3104 # os-win32.c does not
3105 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c'))
3106 softmmu_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')])
3109 common_ss.add(files('cpus-common.c'))
3113 common_ss.add(capstone)
3114 specific_ss.add(files('cpu.c', 'disas.c'), capstone)
3116 # Work around a gcc bug/misfeature wherein constant propagation looks
3118 # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696
3119 # to guess that a const variable is always zero. Without lto, this is
3120 # impossible, as the alias is restricted to page-vary-common.c. Indeed,
3121 # without lto, not even the alias is required -- we simply use different
3122 # declarations in different compilation units.
3123 pagevary = files('page-vary-common.c')
3124 if get_option('b_lto')
3125 pagevary_flags = ['-fno-lto']
3126 if get_option('cfi')
3127 pagevary_flags += '-fno-sanitize=cfi-icall'
3129 pagevary = static_library('page-vary-common', sources: pagevary + genh,
3130 c_args: pagevary_flags)
3131 pagevary = declare_dependency(link_with: pagevary)
3133 common_ss.add(pagevary)
3134 specific_ss.add(files('page-vary.c'))
3142 subdir('semihosting')
3150 common_user_inc = []
3152 subdir('common-user')
3154 subdir('linux-user')
3156 # needed for fuzzing binaries
3157 subdir('tests/qtest/libqos')
3158 subdir('tests/qtest/fuzz')
3161 tcg_real_module_ss = ss.source_set()
3162 tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss)
3163 specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss)
3164 target_modules += { 'accel' : { 'qtest': qtest_module_ss,
3165 'tcg': tcg_real_module_ss }}
3167 ########################
3168 # Library dependencies #
3169 ########################
3171 modinfo_collect = find_program('scripts/modinfo-collect.py')
3172 modinfo_generate = find_program('scripts/modinfo-generate.py')
3177 foreach d, list : modules
3178 foreach m, module_ss : list
3179 if enable_modules and targetos != 'windows'
3180 module_ss = module_ss.apply(config_all, strict: false)
3181 sl = static_library(d + '-' + m, [genh, module_ss.sources()],
3182 dependencies: [modulecommon, module_ss.dependencies()], pic: true)
3188 if module_ss.sources() != []
3189 # FIXME: Should use sl.extract_all_objects(recursive: true) as
3190 # input. Sources can be used multiple times but objects are
3191 # unique when it comes to lookup in compile_commands.json.
3192 # Depnds on a mesion version with
3193 # https://github.com/mesonbuild/meson/pull/8900
3194 modinfo_files += custom_target(d + '-' + m + '.modinfo',
3195 output: d + '-' + m + '.modinfo',
3196 input: module_ss.sources() + genh,
3198 command: [modinfo_collect, module_ss.sources()])
3202 block_ss.add_all(module_ss)
3204 softmmu_ss.add_all(module_ss)
3210 foreach d, list : target_modules
3211 foreach m, module_ss : list
3212 if enable_modules and targetos != 'windows'
3213 foreach target : target_dirs
3214 if target.endswith('-softmmu')
3215 config_target = config_target_mak[target]
3216 config_target += config_host
3217 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3218 c_args = ['-DNEED_CPU_H',
3219 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3220 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3221 target_module_ss = module_ss.apply(config_target, strict: false)
3222 if target_module_ss.sources() != []
3223 module_name = d + '-' + m + '-' + config_target['TARGET_NAME']
3224 sl = static_library(module_name,
3225 [genh, target_module_ss.sources()],
3226 dependencies: [modulecommon, target_module_ss.dependencies()],
3227 include_directories: target_inc,
3231 # FIXME: Should use sl.extract_all_objects(recursive: true) too.
3232 modinfo_files += custom_target(module_name + '.modinfo',
3233 output: module_name + '.modinfo',
3234 input: target_module_ss.sources() + genh,
3236 command: [modinfo_collect, '--target', target, target_module_ss.sources()])
3241 specific_ss.add_all(module_ss)
3247 foreach target : target_dirs
3248 if target.endswith('-softmmu')
3249 config_target = config_target_mak[target]
3250 config_devices_mak = target + '-config-devices.mak'
3251 modinfo_src = custom_target('modinfo-' + target + '.c',
3252 output: 'modinfo-' + target + '.c',
3253 input: modinfo_files,
3254 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'],
3257 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src)
3258 modinfo_dep = declare_dependency(link_with: modinfo_lib)
3260 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH']
3261 hw_arch[arch].add(modinfo_dep)
3266 nm = find_program('nm')
3267 undefsym = find_program('scripts/undefsym.py')
3268 block_syms = custom_target('block.syms', output: 'block.syms',
3269 input: [libqemuutil, block_mods],
3271 command: [undefsym, nm, '@INPUT@'])
3272 qemu_syms = custom_target('qemu.syms', output: 'qemu.syms',
3273 input: [libqemuutil, softmmu_mods],
3275 command: [undefsym, nm, '@INPUT@'])
3277 authz_ss = authz_ss.apply(config_host, strict: false)
3278 libauthz = static_library('authz', authz_ss.sources() + genh,
3279 dependencies: [authz_ss.dependencies()],
3281 build_by_default: false)
3283 authz = declare_dependency(link_whole: libauthz,
3286 crypto_ss = crypto_ss.apply(config_host, strict: false)
3287 libcrypto = static_library('crypto', crypto_ss.sources() + genh,
3288 dependencies: [crypto_ss.dependencies()],
3290 build_by_default: false)
3292 crypto = declare_dependency(link_whole: libcrypto,
3293 dependencies: [authz, qom])
3295 io_ss = io_ss.apply(config_host, strict: false)
3296 libio = static_library('io', io_ss.sources() + genh,
3297 dependencies: [io_ss.dependencies()],
3298 link_with: libqemuutil,
3300 build_by_default: false)
3302 io = declare_dependency(link_whole: libio, dependencies: [crypto, qom])
3304 libmigration = static_library('migration', sources: migration_files + genh,
3306 build_by_default: false)
3307 migration = declare_dependency(link_with: libmigration,
3308 dependencies: [zlib, qom, io])
3309 softmmu_ss.add(migration)
3311 block_ss = block_ss.apply(config_host, strict: false)
3312 libblock = static_library('block', block_ss.sources() + genh,
3313 dependencies: block_ss.dependencies(),
3314 link_depends: block_syms,
3316 build_by_default: false)
3318 block = declare_dependency(link_whole: [libblock],
3319 link_args: '@block.syms',
3320 dependencies: [crypto, io])
3322 blockdev_ss = blockdev_ss.apply(config_host, strict: false)
3323 libblockdev = static_library('blockdev', blockdev_ss.sources() + genh,
3324 dependencies: blockdev_ss.dependencies(),
3326 build_by_default: false)
3328 blockdev = declare_dependency(link_whole: [libblockdev],
3329 dependencies: [block, event_loop_base])
3331 qmp_ss = qmp_ss.apply(config_host, strict: false)
3332 libqmp = static_library('qmp', qmp_ss.sources() + genh,
3333 dependencies: qmp_ss.dependencies(),
3335 build_by_default: false)
3337 qmp = declare_dependency(link_whole: [libqmp])
3339 libchardev = static_library('chardev', chardev_ss.sources() + genh,
3341 dependencies: chardev_ss.dependencies(),
3342 build_by_default: false)
3344 chardev = declare_dependency(link_whole: libchardev)
3346 hwcore_ss = hwcore_ss.apply(config_host, strict: false)
3347 libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh,
3349 build_by_default: false)
3350 hwcore = declare_dependency(link_whole: libhwcore)
3351 common_ss.add(hwcore)
3357 emulator_modules = []
3358 foreach m : block_mods + softmmu_mods
3359 emulator_modules += shared_module(m.name(),
3360 build_by_default: true,
3364 install_dir: qemu_moddir)
3366 if emulator_modules.length() > 0
3367 alias_target('modules', emulator_modules)
3370 softmmu_ss.add(authz, blockdev, chardev, crypto, io, qmp)
3371 common_ss.add(qom, qemuutil)
3373 common_ss.add_all(when: 'CONFIG_SOFTMMU', if_true: [softmmu_ss])
3374 common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss)
3376 common_all = common_ss.apply(config_all, strict: false)
3377 common_all = static_library('common',
3378 build_by_default: false,
3379 sources: common_all.sources() + genh,
3380 include_directories: common_user_inc,
3381 implicit_include_directories: false,
3382 dependencies: common_all.dependencies(),
3385 feature_to_c = find_program('scripts/feature_to_c.sh')
3387 if targetos == 'darwin'
3388 entitlement = find_program('scripts/entitlement.sh')
3392 foreach target : target_dirs
3393 config_target = config_target_mak[target]
3394 target_name = config_target['TARGET_NAME']
3395 target_base_arch = config_target['TARGET_BASE_ARCH']
3396 arch_srcs = [config_target_h[target]]
3398 c_args = ['-DNEED_CPU_H',
3399 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target),
3400 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)]
3401 link_args = emulator_link_args
3403 config_target += config_host
3404 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])]
3405 if targetos == 'linux'
3406 target_inc += include_directories('linux-headers', is_system: true)
3408 if target.endswith('-softmmu')
3409 target_type='system'
3410 t = target_softmmu_arch[target_base_arch].apply(config_target, strict: false)
3411 arch_srcs += t.sources()
3412 arch_deps += t.dependencies()
3414 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch
3415 hw = hw_arch[hw_dir].apply(config_target, strict: false)
3416 arch_srcs += hw.sources()
3417 arch_deps += hw.dependencies()
3419 arch_srcs += config_devices_h[target]
3420 link_args += ['@block.syms', '@qemu.syms']
3422 abi = config_target['TARGET_ABI_DIR']
3424 target_inc += common_user_inc
3425 if target_base_arch in target_user_arch
3426 t = target_user_arch[target_base_arch].apply(config_target, strict: false)
3427 arch_srcs += t.sources()
3428 arch_deps += t.dependencies()
3430 if 'CONFIG_LINUX_USER' in config_target
3431 base_dir = 'linux-user'
3433 if 'CONFIG_BSD_USER' in config_target
3434 base_dir = 'bsd-user'
3435 target_inc += include_directories('bsd-user/' / targetos)
3436 target_inc += include_directories('bsd-user/host/' / host_arch)
3437 dir = base_dir / abi
3438 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c')
3440 target_inc += include_directories(
3444 if 'CONFIG_LINUX_USER' in config_target
3445 dir = base_dir / abi
3446 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c')
3447 if config_target.has_key('TARGET_SYSTBL_ABI')
3449 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'],
3450 extra_args : config_target['TARGET_SYSTBL_ABI'])
3455 if 'TARGET_XML_FILES' in config_target
3456 gdbstub_xml = custom_target(target + '-gdbstub-xml.c',
3457 output: target + '-gdbstub-xml.c',
3458 input: files(config_target['TARGET_XML_FILES'].split()),
3459 command: [feature_to_c, '@INPUT@'],
3461 arch_srcs += gdbstub_xml
3464 t = target_arch[target_base_arch].apply(config_target, strict: false)
3465 arch_srcs += t.sources()
3466 arch_deps += t.dependencies()
3468 target_common = common_ss.apply(config_target, strict: false)
3469 objects = common_all.extract_objects(target_common.sources())
3470 deps = target_common.dependencies()
3472 target_specific = specific_ss.apply(config_target, strict: false)
3473 arch_srcs += target_specific.sources()
3474 arch_deps += target_specific.dependencies()
3476 lib = static_library('qemu-' + target,
3477 sources: arch_srcs + genh,
3478 dependencies: arch_deps,
3480 include_directories: target_inc,
3482 build_by_default: false,
3485 if target.endswith('-softmmu')
3487 'name': 'qemu-system-' + target_name,
3488 'win_subsystem': 'console',
3489 'sources': files('softmmu/main.c'),
3492 if targetos == 'windows' and (sdl.found() or gtk.found())
3494 'name': 'qemu-system-' + target_name + 'w',
3495 'win_subsystem': 'windows',
3496 'sources': files('softmmu/main.c'),
3500 if get_option('fuzzing')
3501 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false)
3503 'name': 'qemu-fuzz-' + target_name,
3504 'win_subsystem': 'console',
3505 'sources': specific_fuzz.sources(),
3506 'dependencies': specific_fuzz.dependencies(),
3511 'name': 'qemu-' + target_name,
3512 'win_subsystem': 'console',
3518 exe_name = exe['name']
3519 if targetos == 'darwin'
3520 exe_name += '-unsigned'
3523 emulator = executable(exe_name, exe['sources'],
3526 dependencies: arch_deps + deps + exe['dependencies'],
3527 objects: lib.extract_all_objects(recursive: true),
3528 link_language: link_language,
3529 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []),
3530 link_args: link_args,
3531 win_subsystem: exe['win_subsystem'])
3533 if targetos == 'darwin'
3534 icon = 'pc-bios/qemu.rsrc'
3535 build_input = [emulator, files(icon)]
3537 get_option('bindir') / exe_name,
3538 meson.current_source_dir() / icon
3540 if 'CONFIG_HVF' in config_target
3541 entitlements = 'accel/hvf/entitlements.plist'
3542 build_input += files(entitlements)
3543 install_input += meson.current_source_dir() / entitlements
3546 emulators += {exe['name'] : custom_target(exe['name'],
3548 output: exe['name'],
3549 command: [entitlement, '@OUTPUT@', '@INPUT@'])
3552 meson.add_install_script(entitlement, '--install',
3553 get_option('bindir') / exe['name'],
3556 emulators += {exe['name']: emulator}
3561 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false},
3562 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true},
3563 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true},
3564 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true},
3566 custom_target(exe['name'] + stp['ext'],
3567 input: trace_events_all,
3568 output: exe['name'] + stp['ext'],
3569 install: stp['install'],
3570 install_dir: get_option('datadir') / 'systemtap/tapset',
3572 tracetool, '--group=all', '--format=' + stp['fmt'],
3573 '--binary=' + stp['bin'],
3574 '--target-name=' + target_name,
3575 '--target-type=' + target_type,
3576 '--probe-prefix=qemu.' + target_type + '.' + target_name,
3577 '@INPUT@', '@OUTPUT@'
3579 depend_files: tracetool_depends)
3585 # Other build targets
3587 if 'CONFIG_PLUGIN' in config_host
3588 install_headers('include/qemu/qemu-plugin.h')
3593 # Don't build qemu-keymap if xkbcommon is not explicitly enabled
3594 # when we don't build tools or system
3595 if xkbcommon.found()
3596 # used for the update-keymaps target, so include rules even if !have_tools
3597 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh,
3598 dependencies: [qemuutil, xkbcommon], install: have_tools)
3602 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep],
3603 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true)
3604 qemu_io = executable('qemu-io', files('qemu-io.c'),
3605 dependencies: [block, qemuutil], install: true)
3606 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'),
3607 dependencies: [blockdev, qemuutil, gnutls, selinux],
3610 subdir('storage-daemon')
3611 subdir('contrib/rdmacm-mux')
3612 subdir('contrib/elf2dmp')
3614 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'),
3615 dependencies: qemuutil,
3619 subdir('contrib/vhost-user-blk')
3620 subdir('contrib/vhost-user-gpu')
3621 subdir('contrib/vhost-user-input')
3622 subdir('contrib/vhost-user-scsi')
3625 if targetos == 'linux'
3626 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'),
3627 dependencies: [qemuutil, libcap_ng],
3629 install_dir: get_option('libexecdir'))
3631 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'),
3632 dependencies: [authz, crypto, io, qom, qemuutil,
3633 libcap_ng, mpathpersist],
3638 subdir('contrib/ivshmem-client')
3639 subdir('contrib/ivshmem-server')
3652 if host_machine.system() == 'windows'
3654 find_program('scripts/nsis.py'),
3656 get_option('prefix'),
3657 meson.current_source_dir(),
3658 config_host['GLIB_BINDIR'],
3661 '-DDISPLAYVERSION=' + meson.project_version(),
3664 nsis_cmd += '-DCONFIG_DOCUMENTATION=y'
3667 nsis_cmd += '-DCONFIG_GTK=y'
3670 nsis = custom_target('nsis',
3671 output: 'qemu-setup-' + meson.project_version() + '.exe',
3672 input: files('qemu.nsi'),
3673 build_always_stale: true,
3674 command: nsis_cmd + ['@INPUT@'])
3675 alias_target('installer', nsis)
3678 #########################
3679 # Configuration summary #
3680 #########################
3684 summary_info += {'Install prefix': get_option('prefix')}
3685 summary_info += {'BIOS directory': qemu_datadir}
3686 pathsep = targetos == 'windows' ? ';' : ':'
3687 summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))}
3688 summary_info += {'binary directory': get_option('prefix') / get_option('bindir')}
3689 summary_info += {'library directory': get_option('prefix') / get_option('libdir')}
3690 summary_info += {'module directory': qemu_moddir}
3691 summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')}
3692 summary_info += {'include directory': get_option('prefix') / get_option('includedir')}
3693 summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')}
3694 if targetos != 'windows'
3695 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')}
3696 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')}
3698 summary_info += {'local state directory': 'queried at runtime'}
3700 summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')}
3701 summary_info += {'Build directory': meson.current_build_dir()}
3702 summary_info += {'Source path': meson.current_source_dir()}
3703 summary_info += {'GIT submodules': config_host['GIT_SUBMODULES']}
3704 summary(summary_info, bool_yn: true, section: 'Directories')
3708 summary_info += {'git': config_host['GIT']}
3709 summary_info += {'make': config_host['MAKE']}
3710 summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())}
3711 summary_info += {'sphinx-build': sphinx_build}
3712 if config_host.has_key('HAVE_GDB_BIN')
3713 summary_info += {'gdb': config_host['HAVE_GDB_BIN']}
3715 summary_info += {'iasl': iasl}
3716 summary_info += {'genisoimage': config_host['GENISOIMAGE']}
3717 if targetos == 'windows' and have_ga
3718 summary_info += {'wixl': wixl}
3720 if slirp.found() and have_system
3721 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false}
3723 summary(summary_info, bool_yn: true, section: 'Host binaries')
3725 # Configurable features
3727 summary_info += {'Documentation': build_docs}
3728 summary_info += {'system-mode emulation': have_system}
3729 summary_info += {'user-mode emulation': have_user}
3730 summary_info += {'block layer': have_block}
3731 summary_info += {'Install blobs': get_option('install_blobs')}
3732 summary_info += {'module support': config_host.has_key('CONFIG_MODULES')}
3733 if config_host.has_key('CONFIG_MODULES')
3734 summary_info += {'alternative module path': get_option('module_upgrades')}
3736 summary_info += {'fuzzing support': get_option('fuzzing')}
3738 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)}
3740 summary_info += {'Trace backends': ','.join(get_option('trace_backends'))}
3741 if 'simple' in get_option('trace_backends')
3742 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'}
3744 summary_info += {'D-Bus display': dbus_display}
3745 summary_info += {'QOM debugging': get_option('qom_cast_debug')}
3746 summary_info += {'vhost-kernel support': have_vhost_kernel}
3747 summary_info += {'vhost-net support': have_vhost_net}
3748 summary_info += {'vhost-user support': have_vhost_user}
3749 summary_info += {'vhost-user-crypto support': have_vhost_user_crypto}
3750 summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server}
3751 summary_info += {'vhost-vdpa support': have_vhost_vdpa}
3752 summary_info += {'build guest agent': have_ga}
3753 summary(summary_info, bool_yn: true, section: 'Configurable features')
3755 # Compilation information
3757 summary_info += {'host CPU': cpu}
3758 summary_info += {'host endianness': build_machine.endian()}
3759 summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())}
3760 summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())}
3761 if link_language == 'cpp'
3762 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())}
3764 summary_info += {'C++ compiler': false}
3766 if targetos == 'darwin'
3767 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())}
3769 option_cflags = (get_option('debug') ? ['-g'] : [])
3770 if get_option('optimization') != 'plain'
3771 option_cflags += ['-O' + get_option('optimization')]
3773 summary_info += {'CFLAGS': ' '.join(get_option('c_args') + option_cflags)}
3774 if link_language == 'cpp'
3775 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args') + option_cflags)}
3777 if targetos == 'darwin'
3778 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args') + option_cflags)}
3780 link_args = get_option(link_language + '_link_args')
3781 if link_args.length() > 0
3782 summary_info += {'LDFLAGS': ' '.join(link_args)}
3784 summary_info += {'QEMU_CFLAGS': ' '.join(qemu_cflags)}
3785 if 'cpp' in all_languages
3786 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_cxxflags)}
3788 if 'objc' in all_languages
3789 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_objcflags)}
3791 summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)}
3792 summary_info += {'profiler': get_option('profiler')}
3793 summary_info += {'link-time optimization (LTO)': get_option('b_lto')}
3794 summary_info += {'PIE': get_option('b_pie')}
3795 summary_info += {'static build': config_host.has_key('CONFIG_STATIC')}
3796 summary_info += {'malloc trim support': has_malloc_trim}
3797 summary_info += {'membarrier': have_membarrier}
3798 summary_info += {'debug stack usage': get_option('debug_stack_usage')}
3799 summary_info += {'mutex debugging': get_option('debug_mutex')}
3800 summary_info += {'memory allocator': get_option('malloc')}
3801 summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')}
3802 summary_info += {'avx512bw optimization': config_host_data.get('CONFIG_AVX512BW_OPT')}
3803 summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')}
3804 if get_option('gprof')
3805 gprof_info = 'YES (deprecated)'
3807 gprof_info = get_option('gprof')
3809 summary_info += {'gprof': gprof_info}
3810 summary_info += {'gcov': get_option('b_coverage')}
3811 summary_info += {'thread sanitizer': config_host.has_key('CONFIG_TSAN')}
3812 summary_info += {'CFI support': get_option('cfi')}
3813 if get_option('cfi')
3814 summary_info += {'CFI debug support': get_option('cfi_debug')}
3816 summary_info += {'strip binaries': get_option('strip')}
3817 summary_info += {'sparse': sparse}
3818 summary_info += {'mingw32 support': targetos == 'windows'}
3819 summary(summary_info, bool_yn: true, section: 'Compilation')
3821 # snarf the cross-compilation information for tests
3824 foreach target: target_dirs
3825 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak'
3826 if fs.exists(tcg_mak)
3827 config_cross_tcg = keyval.load(tcg_mak)
3828 if 'CC' in config_cross_tcg
3829 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']}
3835 summary(summary_info, bool_yn: true, section: 'Cross compilers')
3838 # Targets and accelerators
3841 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')}
3842 summary_info += {'HAX support': config_all.has_key('CONFIG_HAX')}
3843 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')}
3844 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')}
3845 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')}
3846 summary_info += {'Xen support': xen.found()}
3848 summary_info += {'xen ctrl version': xen.version()}
3851 summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')}
3852 if config_all.has_key('CONFIG_TCG')
3853 if get_option('tcg_interpreter')
3854 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'}
3856 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)}
3858 summary_info += {'TCG plugins': config_host.has_key('CONFIG_PLUGIN')}
3859 summary_info += {'TCG debug enabled': config_host.has_key('CONFIG_DEBUG_TCG')}
3861 summary_info += {'target list': ' '.join(target_dirs)}
3863 summary_info += {'default devices': get_option('default_devices')}
3864 summary_info += {'out of process emulation': multiprocess_allowed}
3865 summary_info += {'vfio-user server': vfio_user_server_allowed}
3867 summary(summary_info, bool_yn: true, section: 'Targets and accelerators')
3871 summary_info += {'coroutine backend': config_host['CONFIG_COROUTINE_BACKEND']}
3872 summary_info += {'coroutine pool': have_coroutine_pool}
3874 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')}
3875 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')}
3876 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')}
3877 summary_info += {'VirtFS support': have_virtfs}
3878 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')}
3879 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')}
3880 summary_info += {'bochs support': get_option('bochs').allowed()}
3881 summary_info += {'cloop support': get_option('cloop').allowed()}
3882 summary_info += {'dmg support': get_option('dmg').allowed()}
3883 summary_info += {'qcow v1 support': get_option('qcow1').allowed()}
3884 summary_info += {'vdi support': get_option('vdi').allowed()}
3885 summary_info += {'vvfat support': get_option('vvfat').allowed()}
3886 summary_info += {'qed support': get_option('qed').allowed()}
3887 summary_info += {'parallels support': get_option('parallels').allowed()}
3888 summary_info += {'FUSE exports': fuse}
3889 summary_info += {'VDUSE block exports': have_vduse_blk_export}
3891 summary(summary_info, bool_yn: true, section: 'Block layer support')
3895 summary_info += {'TLS priority': get_option('tls_priority')}
3896 summary_info += {'GNUTLS support': gnutls}
3898 summary_info += {' GNUTLS crypto': gnutls_crypto.found()}
3900 summary_info += {'libgcrypt': gcrypt}
3901 summary_info += {'nettle': nettle}
3903 summary_info += {' XTS': xts != 'private'}
3905 summary_info += {'AF_ALG support': have_afalg}
3906 summary_info += {'rng-none': get_option('rng_none')}
3907 summary_info += {'Linux keyring': have_keyring}
3908 summary(summary_info, bool_yn: true, section: 'Crypto')
3912 if targetos == 'darwin'
3913 summary_info += {'Cocoa support': cocoa}
3914 summary_info += {'vmnet.framework support': vmnet}
3916 summary_info += {'SDL support': sdl}
3917 summary_info += {'SDL image support': sdl_image}
3918 summary_info += {'GTK support': gtk}
3919 summary_info += {'pixman': pixman}
3920 summary_info += {'VTE support': vte}
3921 summary_info += {'slirp support': slirp}
3922 summary_info += {'libtasn1': tasn1}
3923 summary_info += {'PAM': pam}
3924 summary_info += {'iconv support': iconv}
3925 summary_info += {'curses support': curses}
3926 summary_info += {'virgl support': virgl}
3927 summary_info += {'blkio support': blkio}
3928 summary_info += {'curl support': curl}
3929 summary_info += {'Multipath support': mpathpersist}
3930 summary_info += {'PNG support': png}
3931 summary_info += {'VNC support': vnc}
3933 summary_info += {'VNC SASL support': sasl}
3934 summary_info += {'VNC JPEG support': jpeg}
3936 if targetos not in ['darwin', 'haiku', 'windows']
3937 summary_info += {'OSS support': oss}
3938 summary_info += {'sndio support': sndio}
3939 elif targetos == 'darwin'
3940 summary_info += {'CoreAudio support': coreaudio}
3941 elif targetos == 'windows'
3942 summary_info += {'DirectSound support': dsound}
3944 if targetos == 'linux'
3945 summary_info += {'ALSA support': alsa}
3946 summary_info += {'PulseAudio support': pulse}
3948 summary_info += {'JACK support': jack}
3949 summary_info += {'brlapi support': brlapi}
3950 summary_info += {'vde support': vde}
3951 summary_info += {'netmap support': have_netmap}
3952 summary_info += {'l2tpv3 support': have_l2tpv3}
3953 summary_info += {'Linux AIO support': libaio}
3954 summary_info += {'Linux io_uring support': linux_io_uring}
3955 summary_info += {'ATTR/XATTR support': libattr}
3956 summary_info += {'RDMA support': rdma}
3957 summary_info += {'PVRDMA support': have_pvrdma}
3958 summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt}
3959 summary_info += {'libcap-ng support': libcap_ng}
3960 summary_info += {'bpf support': libbpf}
3961 summary_info += {'spice protocol support': spice_protocol}
3962 if spice_protocol.found()
3963 summary_info += {' spice server support': spice}
3965 summary_info += {'rbd support': rbd}
3966 summary_info += {'smartcard support': cacard}
3967 summary_info += {'U2F support': u2f}
3968 summary_info += {'libusb': libusb}
3969 summary_info += {'usb net redir': usbredir}
3970 summary_info += {'OpenGL support (epoxy)': opengl}
3971 summary_info += {'GBM': gbm}
3972 summary_info += {'libiscsi support': libiscsi}
3973 summary_info += {'libnfs support': libnfs}
3974 if targetos == 'windows'
3976 summary_info += {'QGA VSS support': have_qga_vss}
3979 summary_info += {'seccomp support': seccomp}
3980 summary_info += {'GlusterFS support': glusterfs}
3981 summary_info += {'TPM support': have_tpm}
3982 summary_info += {'libssh support': libssh}
3983 summary_info += {'lzo support': lzo}
3984 summary_info += {'snappy support': snappy}
3985 summary_info += {'bzip2 support': libbzip2}
3986 summary_info += {'lzfse support': liblzfse}
3987 summary_info += {'zstd support': zstd}
3988 summary_info += {'NUMA host support': numa}
3989 summary_info += {'capstone': capstone}
3990 summary_info += {'libpmem support': libpmem}
3991 summary_info += {'libdaxctl support': libdaxctl}
3992 summary_info += {'libudev': libudev}
3993 # Dummy dependency, keep .found()
3994 summary_info += {'FUSE lseek': fuse_lseek.found()}
3995 summary_info += {'selinux': selinux}
3996 summary_info += {'libdw': libdw}
3997 summary(summary_info, bool_yn: true, section: 'Dependencies')
3999 if not supported_cpus.contains(cpu)
4001 warning('SUPPORT FOR THIS HOST CPU WILL GO AWAY IN FUTURE RELEASES!')
4003 message('CPU host architecture ' + cpu + ' support is not currently maintained.')
4004 message('The QEMU project intends to remove support for this host CPU in')
4005 message('a future release if nobody volunteers to maintain it and to')
4006 message('provide a build host for our continuous integration setup.')
4007 message('configure has succeeded and you can continue to build, but')
4008 message('if you care about QEMU on this platform you should contact')
4009 message('us upstream at qemu-devel@nongnu.org.')
4012 if not supported_oses.contains(targetos)
4014 warning('WARNING: SUPPORT FOR THIS HOST OS WILL GO AWAY IN FUTURE RELEASES!')
4016 message('Host OS ' + targetos + 'support is not currently maintained.')
4017 message('The QEMU project intends to remove support for this host OS in')
4018 message('a future release if nobody volunteers to maintain it and to')
4019 message('provide a build host for our continuous integration setup.')
4020 message('configure has succeeded and you can continue to build, but')
4021 message('if you care about QEMU on this platform you should contact')
4022 message('us upstream at qemu-devel@nongnu.org.')