1project('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')) 5 6add_test_setup('quick', exclude_suites: ['slow', 'thorough'], is_default: true) 7add_test_setup('slow', exclude_suites: ['thorough'], env: ['G_TEST_SLOW=1', 'SPEED=slow']) 8add_test_setup('thorough', env: ['G_TEST_SLOW=1', 'SPEED=thorough']) 9 10meson.add_postconf_script(find_program('scripts/symlink-install-tree.py')) 11 12not_found = dependency('', required: false) 13keyval = import('keyval') 14ss = import('sourceset') 15fs = import('fs') 16 17targetos = host_machine.system() 18sh = find_program('sh') 19config_host = keyval.load(meson.current_build_dir() / 'config-host.mak') 20enable_modules = 'CONFIG_MODULES' in config_host 21enable_static = 'CONFIG_STATIC' in config_host 22 23# Allow both shared and static libraries unless --enable-static 24static_kwargs = enable_static ? {'static': true} : {} 25 26cc = meson.get_compiler('c') 27all_languages = ['c'] 28if add_languages('cpp', required: false, native: false) 29 all_languages += ['cpp'] 30 cxx = meson.get_compiler('cpp') 31endif 32if targetos == 'darwin' and \ 33 add_languages('objc', required: get_option('cocoa'), native: false) 34 all_languages += ['objc'] 35 objc = meson.get_compiler('objc') 36endif 37 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.) 43tmpdir = meson.current_build_dir() / 'meson-private/temp' 44 45if get_option('qemu_suffix').startswith('/') 46 error('qemu_suffix cannot start with a /') 47endif 48 49qemu_confdir = get_option('sysconfdir') / get_option('qemu_suffix') 50qemu_datadir = get_option('datadir') / get_option('qemu_suffix') 51qemu_docdir = get_option('docdir') / get_option('qemu_suffix') 52qemu_moddir = get_option('libdir') / get_option('qemu_suffix') 53 54qemu_desktopdir = get_option('datadir') / 'applications' 55qemu_icondir = get_option('datadir') / 'icons' 56 57config_host_data = configuration_data() 58genh = [] 59qapi_trace_events = [] 60 61bsd_oses = ['gnu/kfreebsd', 'freebsd', 'netbsd', 'openbsd', 'dragonfly', 'darwin'] 62supported_oses = ['windows', 'freebsd', 'netbsd', 'openbsd', 'darwin', 'sunos', 'linux'] 63supported_cpus = ['ppc', 'ppc64', 's390x', 'riscv', 'x86', 'x86_64', 64 'arm', 'aarch64', 'loongarch64', 'mips', 'mips64', 'sparc64'] 65 66cpu = host_machine.cpu_family() 67 68# Unify riscv* to a single family. 69if cpu in ['riscv32', 'riscv64'] 70 cpu = 'riscv' 71endif 72 73target_dirs = config_host['TARGET_DIRS'].split() 74have_linux_user = false 75have_bsd_user = false 76have_system = false 77foreach 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') 81endforeach 82have_user = have_linux_user or have_bsd_user 83have_tools = get_option('tools') \ 84 .disable_auto_if(not have_system) \ 85 .allowed() 86have_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') \ 90 .allowed() 91have_block = have_system or have_tools 92 93python = import('python').find_installation() 94 95if cpu not in supported_cpus 96 host_arch = 'unknown' 97elif cpu == 'x86' 98 host_arch = 'i386' 99elif cpu == 'mips64' 100 host_arch = 'mips' 101else 102 host_arch = cpu 103endif 104 105if cpu in ['x86', 'x86_64'] 106 kvm_targets = ['i386-softmmu', 'x86_64-softmmu'] 107elif cpu == 'aarch64' 108 kvm_targets = ['aarch64-softmmu'] 109elif cpu == 's390x' 110 kvm_targets = ['s390x-softmmu'] 111elif cpu in ['ppc', 'ppc64'] 112 kvm_targets = ['ppc-softmmu', 'ppc64-softmmu'] 113elif cpu in ['mips', 'mips64'] 114 kvm_targets = ['mips-softmmu', 'mipsel-softmmu', 'mips64-softmmu', 'mips64el-softmmu'] 115elif cpu in ['riscv'] 116 kvm_targets = ['riscv32-softmmu', 'riscv64-softmmu'] 117else 118 kvm_targets = [] 119endif 120 121kvm_targets_c = '""' 122if get_option('kvm').allowed() and targetos == 'linux' 123 kvm_targets_c = '"' + '" ,"'.join(kvm_targets) + '"' 124endif 125config_host_data.set('CONFIG_KVM_TARGETS', kvm_targets_c) 126 127accelerator_targets = { 'CONFIG_KVM': kvm_targets } 128 129if cpu in ['aarch64'] 130 accelerator_targets += { 131 'CONFIG_HVF': ['aarch64-softmmu'] 132 } 133endif 134 135if 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'], 139 } 140endif 141if 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'], 147 } 148endif 149 150modular_tcg = [] 151# Darwin does not support references to thread-local variables in modules 152if targetos != 'darwin' 153 modular_tcg = ['i386-softmmu', 'x86_64-softmmu'] 154endif 155 156edk2_targets = [ 'arm-softmmu', 'aarch64-softmmu', 'i386-softmmu', 'x86_64-softmmu' ] 157unpack_edk2_blobs = false 158foreach 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() 162 break 163 endif 164endforeach 165 166dtrace = not_found 167stap = not_found 168if 'dtrace' in get_option('trace_backends') 169 dtrace = find_program('dtrace', required: true) 170 stap = find_program('stap', required: false) 171 if stap.found() 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 176 # object. 177 add_global_arguments('-DSTAP_SDT_V2', 178 native: false, language: all_languages) 179 endif 180endif 181 182if get_option('iasl') == '' 183 iasl = find_program('iasl', required: false) 184else 185 iasl = find_program(get_option('iasl'), required: true) 186endif 187 188################## 189# Compiler flags # 190################## 191 192qemu_cflags = config_host['QEMU_CFLAGS'].split() 193qemu_objcflags = config_host['QEMU_OBJCFLAGS'].split() 194qemu_ldflags = config_host['QEMU_LDFLAGS'].split() 195 196if enable_static 197 qemu_ldflags += get_option('b_pie') ? '-static-pie' : '-static' 198endif 199 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. 202qemu_ldflags += cc.get_supported_link_arguments('-Wl,-z,relro', '-Wl,-z,now') 203 204if 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') 207endif 208 209if get_option('gprof') 210 qemu_cflags += ['-p'] 211 qemu_objcflags += ['-p'] 212 qemu_ldflags += ['-p'] 213endif 214 215# Specify linker-script with add_project_link_arguments so that it is not placed 216# within a linker --start-group/--end-group pair 217if get_option('fuzzing') 218 add_project_link_arguments(['-Wl,-T,', 219 (meson.current_source_dir() / 'tests/qtest/fuzz/fork_fuzz.ld')], 220 native: false, language: all_languages) 221 222 # Specify a filter to only instrument code that is directly related to 223 # virtual-devices. 224 configure_file(output: 'instrumentation-filter', 225 input: 'scripts/oss-fuzz/instrumentation-filter-template', 226 copy: true) 227 228 if cc.compiles('int main () { return 0; }', 229 name: '-fsanitize-coverage-allowlist=/dev/null', 230 args: ['-fsanitize-coverage-allowlist=/dev/null', 231 '-fsanitize-coverage=trace-pc'] ) 232 add_global_arguments('-fsanitize-coverage-allowlist=instrumentation-filter', 233 native: false, language: all_languages) 234 endif 235 236 if get_option('fuzzing_engine') == '' 237 # Add CFLAGS to tell clang to add fuzzer-related instrumentation to all the 238 # compiled code. To build non-fuzzer binaries with --enable-fuzzing, link 239 # everything with fsanitize=fuzzer-no-link. Otherwise, the linker will be 240 # unable to bind the fuzzer-related callbacks added by instrumentation. 241 add_global_arguments('-fsanitize=fuzzer-no-link', 242 native: false, language: all_languages) 243 add_global_link_arguments('-fsanitize=fuzzer-no-link', 244 native: false, language: all_languages) 245 # For the actual fuzzer binaries, we need to link against the libfuzzer 246 # library. They need to be configurable, to support OSS-Fuzz 247 fuzz_exe_ldflags = ['-fsanitize=fuzzer'] 248 else 249 # LIB_FUZZING_ENGINE was set; assume we are running on OSS-Fuzz, and 250 # the needed CFLAGS have already been provided 251 fuzz_exe_ldflags = get_option('fuzzing_engine').split() 252 endif 253endif 254 255# Check that the C++ compiler exists and works with the C compiler. 256link_language = 'c' 257linker = cc 258qemu_cxxflags = [] 259if 'cpp' in all_languages 260 add_global_arguments(['-D__STDC_LIMIT_MACROS', '-D__STDC_CONSTANT_MACROS', '-D__STDC_FORMAT_MACROS'], 261 native: false, language: 'cpp') 262 foreach k: qemu_cflags 263 if k not in ['-Wstrict-prototypes', '-Wmissing-prototypes', '-Wnested-externs', 264 '-Wold-style-declaration', '-Wold-style-definition', '-Wredundant-decls'] 265 qemu_cxxflags += [k] 266 endif 267 endforeach 268 269 if cxx.links(files('scripts/main.c'), args: qemu_cflags) 270 link_language = 'cpp' 271 linker = cxx 272 else 273 message('C++ compiler does not work with C compiler') 274 message('Disabling C++-specific optional code') 275 endif 276endif 277 278# Exclude --warn-common with TSan to suppress warnings from the TSan libraries. 279if targetos != 'sunos' and not config_host.has_key('CONFIG_TSAN') 280 qemu_ldflags += linker.get_supported_link_arguments('-Wl,--warn-common') 281endif 282 283add_global_link_arguments(qemu_ldflags, native: false, language: all_languages) 284 285add_global_arguments(qemu_cflags, native: false, language: 'c') 286add_global_arguments(qemu_cxxflags, native: false, language: 'cpp') 287add_global_arguments(qemu_objcflags, native: false, language: 'objc') 288if targetos == 'linux' 289 add_project_arguments('-isystem', meson.current_source_dir() / 'linux-headers', 290 '-isystem', 'linux-headers', 291 language: all_languages) 292endif 293 294add_project_arguments('-iquote', '.', 295 '-iquote', meson.current_source_dir(), 296 '-iquote', meson.current_source_dir() / 'include', 297 language: all_languages) 298 299sparse = find_program('cgcc', required: get_option('sparse')) 300if sparse.found() 301 run_target('sparse', 302 command: [find_program('scripts/check_sparse.py'), 303 'compile_commands.json', sparse.full_path(), '-Wbitwise', 304 '-Wno-transparent-union', '-Wno-old-initializer', 305 '-Wno-non-pointer-null']) 306endif 307 308########################################### 309# Target-specific checks and dependencies # 310########################################### 311 312# Fuzzing 313if get_option('fuzzing') and get_option('fuzzing_engine') == '' and \ 314 not cc.links(''' 315 #include <stdint.h> 316 #include <sys/types.h> 317 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size); 318 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; } 319 ''', 320 args: ['-Werror', '-fsanitize=fuzzer']) 321 error('Your compiler does not support -fsanitize=fuzzer') 322endif 323 324# Tracing backends 325if 'ftrace' in get_option('trace_backends') and targetos != 'linux' 326 error('ftrace is supported only on Linux') 327endif 328if 'syslog' in get_option('trace_backends') and not cc.compiles(''' 329 #include <syslog.h> 330 int main(void) { 331 openlog("qemu", LOG_PID, LOG_DAEMON); 332 syslog(LOG_INFO, "configure"); 333 return 0; 334 }''') 335 error('syslog is not supported on this system') 336endif 337 338# Miscellaneous Linux-only features 339get_option('mpath') \ 340 .require(targetos == 'linux', error_message: 'Multipath is supported only on Linux') 341 342multiprocess_allowed = get_option('multiprocess') \ 343 .require(targetos == 'linux', error_message: 'Multiprocess QEMU is supported only on Linux') \ 344 .allowed() 345 346vfio_user_server_allowed = get_option('vfio_user_server') \ 347 .require(targetos == 'linux', error_message: 'vfio-user server is supported only on Linux') \ 348 .allowed() 349 350have_tpm = get_option('tpm') \ 351 .require(targetos != 'windows', error_message: 'TPM emulation only available on POSIX systems') \ 352 .allowed() 353 354# vhost 355have_vhost_user = get_option('vhost_user') \ 356 .disable_auto_if(targetos != 'linux') \ 357 .require(targetos != 'windows', 358 error_message: 'vhost-user is not available on Windows').allowed() 359have_vhost_vdpa = get_option('vhost_vdpa') \ 360 .require(targetos == 'linux', 361 error_message: 'vhost-vdpa is only available on Linux').allowed() 362have_vhost_kernel = get_option('vhost_kernel') \ 363 .require(targetos == 'linux', 364 error_message: 'vhost-kernel is only available on Linux').allowed() 365have_vhost_user_crypto = get_option('vhost_crypto') \ 366 .require(have_vhost_user, 367 error_message: 'vhost-crypto requires vhost-user to be enabled').allowed() 368 369have_vhost = have_vhost_user or have_vhost_vdpa or have_vhost_kernel 370 371have_vhost_net_user = have_vhost_user and get_option('vhost_net').allowed() 372have_vhost_net_vdpa = have_vhost_vdpa and get_option('vhost_net').allowed() 373have_vhost_net_kernel = have_vhost_kernel and get_option('vhost_net').allowed() 374have_vhost_net = have_vhost_net_kernel or have_vhost_net_user or have_vhost_net_vdpa 375 376# Target-specific libraries and flags 377libm = cc.find_library('m', required: false) 378threads = dependency('threads') 379util = cc.find_library('util', required: false) 380winmm = [] 381socket = [] 382version_res = [] 383coref = [] 384iokit = [] 385emulator_link_args = [] 386nvmm =not_found 387hvf = not_found 388midl = not_found 389widl = not_found 390pathcch = not_found 391host_dsosuf = '.so' 392if targetos == 'windows' 393 midl = find_program('midl', required: false) 394 widl = find_program('widl', required: false) 395 pathcch = cc.find_library('pathcch') 396 socket = cc.find_library('ws2_32') 397 winmm = cc.find_library('winmm') 398 399 win = import('windows') 400 version_res = win.compile_resources('version.rc', 401 depend_files: files('pc-bios/qemu-nsis.ico'), 402 include_directories: include_directories('.')) 403 host_dsosuf = '.dll' 404elif targetos == 'darwin' 405 coref = dependency('appleframeworks', modules: 'CoreFoundation') 406 iokit = dependency('appleframeworks', modules: 'IOKit', required: false) 407 host_dsosuf = '.dylib' 408elif targetos == 'sunos' 409 socket = [cc.find_library('socket'), 410 cc.find_library('nsl'), 411 cc.find_library('resolv')] 412elif targetos == 'haiku' 413 socket = [cc.find_library('posix_error_mapper'), 414 cc.find_library('network'), 415 cc.find_library('bsd')] 416elif targetos == 'openbsd' 417 if get_option('tcg').allowed() and target_dirs.length() > 0 418 # Disable OpenBSD W^X if available 419 emulator_link_args = cc.get_supported_link_arguments('-Wl,-z,wxneeded') 420 endif 421endif 422 423# Target-specific configuration of accelerators 424accelerators = [] 425if get_option('kvm').allowed() and targetos == 'linux' 426 accelerators += 'CONFIG_KVM' 427endif 428if get_option('whpx').allowed() and targetos == 'windows' 429 if get_option('whpx').enabled() and host_machine.cpu() != 'x86_64' 430 error('WHPX requires 64-bit host') 431 elif cc.has_header('WinHvPlatform.h', required: get_option('whpx')) and \ 432 cc.has_header('WinHvEmulation.h', required: get_option('whpx')) 433 accelerators += 'CONFIG_WHPX' 434 endif 435endif 436if get_option('hvf').allowed() 437 hvf = dependency('appleframeworks', modules: 'Hypervisor', 438 required: get_option('hvf')) 439 if hvf.found() 440 accelerators += 'CONFIG_HVF' 441 endif 442endif 443if get_option('hax').allowed() 444 if get_option('hax').enabled() or targetos in ['windows', 'darwin', 'netbsd'] 445 accelerators += 'CONFIG_HAX' 446 endif 447endif 448if targetos == 'netbsd' 449 nvmm = cc.find_library('nvmm', required: get_option('nvmm')) 450 if nvmm.found() 451 accelerators += 'CONFIG_NVMM' 452 endif 453endif 454 455tcg_arch = host_arch 456if get_option('tcg').allowed() 457 if host_arch == 'unknown' 458 if get_option('tcg_interpreter') 459 warning('Unsupported CPU @0@, will use TCG with TCI (slow)'.format(cpu)) 460 else 461 error('Unsupported CPU @0@, try --enable-tcg-interpreter'.format(cpu)) 462 endif 463 elif get_option('tcg_interpreter') 464 warning('Use of the TCG interpreter is not recommended on this host') 465 warning('architecture. There is a native TCG execution backend available') 466 warning('which provides substantially better performance and reliability.') 467 warning('It is strongly recommended to remove the --enable-tcg-interpreter') 468 warning('configuration option on this architecture to use the native') 469 warning('backend.') 470 endif 471 if get_option('tcg_interpreter') 472 tcg_arch = 'tci' 473 config_host += { 'CONFIG_TCG_INTERPRETER': 'y' } 474 elif host_arch == 'x86_64' 475 tcg_arch = 'i386' 476 elif host_arch == 'ppc64' 477 tcg_arch = 'ppc' 478 endif 479 add_project_arguments('-iquote', meson.current_source_dir() / 'tcg' / tcg_arch, 480 language: all_languages) 481 482 accelerators += 'CONFIG_TCG' 483 config_host += { 'CONFIG_TCG': 'y' } 484endif 485 486if 'CONFIG_KVM' not in accelerators and get_option('kvm').enabled() 487 error('KVM not available on this platform') 488endif 489if 'CONFIG_HVF' not in accelerators and get_option('hvf').enabled() 490 error('HVF not available on this platform') 491endif 492if 'CONFIG_NVMM' not in accelerators and get_option('nvmm').enabled() 493 error('NVMM not available on this platform') 494endif 495if 'CONFIG_WHPX' not in accelerators and get_option('whpx').enabled() 496 error('WHPX not available on this platform') 497endif 498 499################ 500# Dependencies # 501################ 502 503# The path to glib.h is added to all compilation commands. This was 504# grandfathered in from the QEMU Makefiles. 505add_project_arguments(config_host['GLIB_CFLAGS'].split(), 506 native: false, language: all_languages) 507glib = declare_dependency(compile_args: config_host['GLIB_CFLAGS'].split(), 508 link_args: config_host['GLIB_LIBS'].split(), 509 version: config_host['GLIB_VERSION'], 510 variables: { 511 'bindir': config_host['GLIB_BINDIR'], 512 }) 513# override glib dep with the configure results (for subprojects) 514meson.override_dependency('glib-2.0', glib) 515 516gio = not_found 517gdbus_codegen = not_found 518gdbus_codegen_error = '@0@ requires gdbus-codegen, please install libgio' 519if not get_option('gio').auto() or have_system 520 gio = dependency('gio-2.0', required: get_option('gio'), 521 method: 'pkg-config', kwargs: static_kwargs) 522 if gio.found() and not cc.links(''' 523 #include <gio/gio.h> 524 int main(void) 525 { 526 g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0); 527 return 0; 528 }''', dependencies: [glib, gio]) 529 if get_option('gio').enabled() 530 error('The installed libgio is broken for static linking') 531 endif 532 gio = not_found 533 endif 534 if gio.found() 535 gdbus_codegen = find_program(gio.get_variable('gdbus_codegen'), 536 required: get_option('gio')) 537 gio_unix = dependency('gio-unix-2.0', required: get_option('gio'), 538 method: 'pkg-config', kwargs: static_kwargs) 539 gio = declare_dependency(dependencies: [gio, gio_unix], 540 version: gio.version()) 541 endif 542endif 543if gdbus_codegen.found() and get_option('cfi') 544 gdbus_codegen = not_found 545 gdbus_codegen_error = '@0@ uses gdbus-codegen, which does not support control flow integrity' 546endif 547 548lttng = not_found 549if 'ust' in get_option('trace_backends') 550 lttng = dependency('lttng-ust', required: true, version: '>= 2.1', 551 method: 'pkg-config', kwargs: static_kwargs) 552endif 553pixman = not_found 554if have_system or have_tools 555 pixman = dependency('pixman-1', required: have_system, version:'>=0.21.8', 556 method: 'pkg-config', kwargs: static_kwargs) 557endif 558zlib = dependency('zlib', required: true, kwargs: static_kwargs) 559 560libaio = not_found 561if not get_option('linux_aio').auto() or have_block 562 libaio = cc.find_library('aio', has_headers: ['libaio.h'], 563 required: get_option('linux_aio'), 564 kwargs: static_kwargs) 565endif 566 567linux_io_uring_test = ''' 568 #include <liburing.h> 569 #include <linux/errqueue.h> 570 571 int main(void) { return 0; }''' 572 573linux_io_uring = not_found 574if not get_option('linux_io_uring').auto() or have_block 575 linux_io_uring = dependency('liburing', version: '>=0.3', 576 required: get_option('linux_io_uring'), 577 method: 'pkg-config', kwargs: static_kwargs) 578 if not cc.links(linux_io_uring_test) 579 linux_io_uring = not_found 580 endif 581endif 582 583libnfs = not_found 584if not get_option('libnfs').auto() or have_block 585 libnfs = dependency('libnfs', version: '>=1.9.3', 586 required: get_option('libnfs'), 587 method: 'pkg-config', kwargs: static_kwargs) 588endif 589 590libattr_test = ''' 591 #include <stddef.h> 592 #include <sys/types.h> 593 #ifdef CONFIG_LIBATTR 594 #include <attr/xattr.h> 595 #else 596 #include <sys/xattr.h> 597 #endif 598 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }''' 599 600libattr = not_found 601have_old_libattr = false 602if get_option('attr').allowed() 603 if cc.links(libattr_test) 604 libattr = declare_dependency() 605 else 606 libattr = cc.find_library('attr', has_headers: ['attr/xattr.h'], 607 required: get_option('attr'), 608 kwargs: static_kwargs) 609 if libattr.found() and not \ 610 cc.links(libattr_test, dependencies: libattr, args: '-DCONFIG_LIBATTR') 611 libattr = not_found 612 if get_option('attr').enabled() 613 error('could not link libattr') 614 else 615 warning('could not link libattr, disabling') 616 endif 617 else 618 have_old_libattr = libattr.found() 619 endif 620 endif 621endif 622 623cocoa = dependency('appleframeworks', modules: ['Cocoa', 'CoreVideo'], 624 required: get_option('cocoa')) 625 626vmnet = dependency('appleframeworks', modules: 'vmnet', required: get_option('vmnet')) 627if vmnet.found() and not cc.has_header_symbol('vmnet/vmnet.h', 628 'VMNET_BRIDGED_MODE', 629 dependencies: vmnet) 630 vmnet = not_found 631 if get_option('vmnet').enabled() 632 error('vmnet.framework API is outdated') 633 else 634 warning('vmnet.framework API is outdated, disabling') 635 endif 636endif 637 638seccomp = not_found 639seccomp_has_sysrawrc = false 640if not get_option('seccomp').auto() or have_system or have_tools 641 seccomp = dependency('libseccomp', version: '>=2.3.0', 642 required: get_option('seccomp'), 643 method: 'pkg-config', kwargs: static_kwargs) 644 if seccomp.found() 645 seccomp_has_sysrawrc = cc.has_header_symbol('seccomp.h', 646 'SCMP_FLTATR_API_SYSRAWRC', 647 dependencies: seccomp) 648 endif 649endif 650 651libcap_ng = not_found 652if not get_option('cap_ng').auto() or have_system or have_tools 653 libcap_ng = cc.find_library('cap-ng', has_headers: ['cap-ng.h'], 654 required: get_option('cap_ng'), 655 kwargs: static_kwargs) 656endif 657if libcap_ng.found() and not cc.links(''' 658 #include <cap-ng.h> 659 int main(void) 660 { 661 capng_capability_to_name(CAPNG_EFFECTIVE); 662 return 0; 663 }''', dependencies: libcap_ng) 664 libcap_ng = not_found 665 if get_option('cap_ng').enabled() 666 error('could not link libcap-ng') 667 else 668 warning('could not link libcap-ng, disabling') 669 endif 670endif 671 672if get_option('xkbcommon').auto() and not have_system and not have_tools 673 xkbcommon = not_found 674else 675 xkbcommon = dependency('xkbcommon', required: get_option('xkbcommon'), 676 method: 'pkg-config', kwargs: static_kwargs) 677endif 678 679slirp = not_found 680if not get_option('slirp').auto() or have_system 681 slirp = dependency('slirp', required: get_option('slirp'), 682 method: 'pkg-config', kwargs: static_kwargs) 683 # slirp < 4.7 is incompatible with CFI support in QEMU. This is because 684 # it passes function pointers within libslirp as callbacks for timers. 685 # When using a system-wide shared libslirp, the type information for the 686 # callback is missing and the timer call produces a false positive with CFI. 687 # Do not use the "version" keyword argument to produce a better error. 688 # with control-flow integrity. 689 if get_option('cfi') and slirp.found() and slirp.version().version_compare('<4.7') 690 if get_option('slirp').enabled() 691 error('Control-Flow Integrity requires libslirp 4.7.') 692 else 693 warning('Cannot use libslirp since Control-Flow Integrity requires libslirp >= 4.7.') 694 slirp = not_found 695 endif 696 endif 697endif 698 699vde = not_found 700if not get_option('vde').auto() or have_system or have_tools 701 vde = cc.find_library('vdeplug', has_headers: ['libvdeplug.h'], 702 required: get_option('vde'), 703 kwargs: static_kwargs) 704endif 705if vde.found() and not cc.links(''' 706 #include <libvdeplug.h> 707 int main(void) 708 { 709 struct vde_open_args a = {0, 0, 0}; 710 char s[] = ""; 711 vde_open(s, s, &a); 712 return 0; 713 }''', dependencies: vde) 714 vde = not_found 715 if get_option('cap_ng').enabled() 716 error('could not link libvdeplug') 717 else 718 warning('could not link libvdeplug, disabling') 719 endif 720endif 721 722pulse = not_found 723if not get_option('pa').auto() or (targetos == 'linux' and have_system) 724 pulse = dependency('libpulse', required: get_option('pa'), 725 method: 'pkg-config', kwargs: static_kwargs) 726endif 727alsa = not_found 728if not get_option('alsa').auto() or (targetos == 'linux' and have_system) 729 alsa = dependency('alsa', required: get_option('alsa'), 730 method: 'pkg-config', kwargs: static_kwargs) 731endif 732jack = not_found 733if not get_option('jack').auto() or have_system 734 jack = dependency('jack', required: get_option('jack'), 735 method: 'pkg-config', kwargs: static_kwargs) 736endif 737sndio = not_found 738if not get_option('sndio').auto() or have_system 739 sndio = dependency('sndio', required: get_option('sndio'), 740 method: 'pkg-config', kwargs: static_kwargs) 741endif 742 743spice_protocol = not_found 744if not get_option('spice_protocol').auto() or have_system 745 spice_protocol = dependency('spice-protocol', version: '>=0.14.0', 746 required: get_option('spice_protocol'), 747 method: 'pkg-config', kwargs: static_kwargs) 748endif 749spice = not_found 750if not get_option('spice').auto() or have_system 751 spice = dependency('spice-server', version: '>=0.14.0', 752 required: get_option('spice'), 753 method: 'pkg-config', kwargs: static_kwargs) 754endif 755spice_headers = spice.partial_dependency(compile_args: true, includes: true) 756 757rt = cc.find_library('rt', required: false) 758 759libiscsi = not_found 760if not get_option('libiscsi').auto() or have_block 761 libiscsi = dependency('libiscsi', version: '>=1.9.0', 762 required: get_option('libiscsi'), 763 method: 'pkg-config', kwargs: static_kwargs) 764endif 765zstd = not_found 766if not get_option('zstd').auto() or have_block 767 zstd = dependency('libzstd', version: '>=1.4.0', 768 required: get_option('zstd'), 769 method: 'pkg-config', kwargs: static_kwargs) 770endif 771virgl = not_found 772 773have_vhost_user_gpu = have_tools and targetos == 'linux' and pixman.found() 774if not get_option('virglrenderer').auto() or have_system or have_vhost_user_gpu 775 virgl = dependency('virglrenderer', 776 method: 'pkg-config', 777 required: get_option('virglrenderer'), 778 kwargs: static_kwargs) 779endif 780blkio = not_found 781if not get_option('blkio').auto() or have_block 782 blkio = dependency('blkio', 783 method: 'pkg-config', 784 required: get_option('blkio'), 785 kwargs: static_kwargs) 786endif 787curl = not_found 788if not get_option('curl').auto() or have_block 789 curl = dependency('libcurl', version: '>=7.29.0', 790 method: 'pkg-config', 791 required: get_option('curl'), 792 kwargs: static_kwargs) 793endif 794libudev = not_found 795if targetos == 'linux' and (have_system or have_tools) 796 libudev = dependency('libudev', 797 method: 'pkg-config', 798 required: get_option('libudev'), 799 kwargs: static_kwargs) 800endif 801 802mpathlibs = [libudev] 803mpathpersist = not_found 804mpathpersist_new_api = false 805if targetos == 'linux' and have_tools and get_option('mpath').allowed() 806 mpath_test_source_new = ''' 807 #include <libudev.h> 808 #include <mpath_persist.h> 809 unsigned mpath_mx_alloc_len = 1024; 810 int logsink; 811 static struct config *multipath_conf; 812 extern struct udev *udev; 813 extern struct config *get_multipath_config(void); 814 extern void put_multipath_config(struct config *conf); 815 struct udev *udev; 816 struct config *get_multipath_config(void) { return multipath_conf; } 817 void put_multipath_config(struct config *conf) { } 818 int main(void) { 819 udev = udev_new(); 820 multipath_conf = mpath_lib_init(); 821 return 0; 822 }''' 823 mpath_test_source_old = ''' 824 #include <libudev.h> 825 #include <mpath_persist.h> 826 unsigned mpath_mx_alloc_len = 1024; 827 int logsink; 828 int main(void) { 829 struct udev *udev = udev_new(); 830 mpath_lib_init(udev); 831 return 0; 832 }''' 833 libmpathpersist = cc.find_library('mpathpersist', 834 required: get_option('mpath'), 835 kwargs: static_kwargs) 836 if libmpathpersist.found() 837 mpathlibs += libmpathpersist 838 if enable_static 839 mpathlibs += cc.find_library('devmapper', 840 required: get_option('mpath'), 841 kwargs: static_kwargs) 842 endif 843 mpathlibs += cc.find_library('multipath', 844 required: get_option('mpath'), 845 kwargs: static_kwargs) 846 foreach lib: mpathlibs 847 if not lib.found() 848 mpathlibs = [] 849 break 850 endif 851 endforeach 852 if mpathlibs.length() == 0 853 msg = 'Dependencies missing for libmpathpersist' 854 elif cc.links(mpath_test_source_new, dependencies: mpathlibs) 855 mpathpersist = declare_dependency(dependencies: mpathlibs) 856 mpathpersist_new_api = true 857 elif cc.links(mpath_test_source_old, dependencies: mpathlibs) 858 mpathpersist = declare_dependency(dependencies: mpathlibs) 859 else 860 msg = 'Cannot detect libmpathpersist API' 861 endif 862 if not mpathpersist.found() 863 if get_option('mpath').enabled() 864 error(msg) 865 else 866 warning(msg + ', disabling') 867 endif 868 endif 869 endif 870endif 871 872iconv = not_found 873curses = not_found 874if have_system and get_option('curses').allowed() 875 curses_test = ''' 876 #if defined(__APPLE__) || defined(__OpenBSD__) 877 #define _XOPEN_SOURCE_EXTENDED 1 878 #endif 879 #include <locale.h> 880 #include <curses.h> 881 #include <wchar.h> 882 int main(void) { 883 wchar_t wch = L'w'; 884 setlocale(LC_ALL, ""); 885 resize_term(0, 0); 886 addwstr(L"wide chars\n"); 887 addnwstr(&wch, 1); 888 add_wch(WACS_DEGREE); 889 return 0; 890 }''' 891 892 curses_dep_list = targetos == 'windows' ? ['ncurses', 'ncursesw'] : ['ncursesw'] 893 curses = dependency(curses_dep_list, 894 required: false, 895 method: 'pkg-config', 896 kwargs: static_kwargs) 897 msg = get_option('curses').enabled() ? 'curses library not found' : '' 898 curses_compile_args = ['-DNCURSES_WIDECHAR=1'] 899 if curses.found() 900 if cc.links(curses_test, args: curses_compile_args, dependencies: [curses]) 901 curses = declare_dependency(compile_args: curses_compile_args, dependencies: [curses]) 902 else 903 msg = 'curses package not usable' 904 curses = not_found 905 endif 906 endif 907 if not curses.found() 908 has_curses_h = cc.has_header('curses.h', args: curses_compile_args) 909 if targetos != 'windows' and not has_curses_h 910 message('Trying with /usr/include/ncursesw') 911 curses_compile_args += ['-I/usr/include/ncursesw'] 912 has_curses_h = cc.has_header('curses.h', args: curses_compile_args) 913 endif 914 if has_curses_h 915 curses_libname_list = (targetos == 'windows' ? ['pdcurses'] : ['ncursesw', 'cursesw']) 916 foreach curses_libname : curses_libname_list 917 libcurses = cc.find_library(curses_libname, 918 required: false, 919 kwargs: static_kwargs) 920 if libcurses.found() 921 if cc.links(curses_test, args: curses_compile_args, dependencies: libcurses) 922 curses = declare_dependency(compile_args: curses_compile_args, 923 dependencies: [libcurses]) 924 break 925 else 926 msg = 'curses library not usable' 927 endif 928 endif 929 endforeach 930 endif 931 endif 932 if get_option('iconv').allowed() 933 foreach link_args : [ ['-liconv'], [] ] 934 # Programs will be linked with glib and this will bring in libiconv on FreeBSD. 935 # We need to use libiconv if available because mixing libiconv's headers with 936 # the system libc does not work. 937 # However, without adding glib to the dependencies -L/usr/local/lib will not be 938 # included in the command line and libiconv will not be found. 939 if cc.links(''' 940 #include <iconv.h> 941 int main(void) { 942 iconv_t conv = iconv_open("WCHAR_T", "UCS-2"); 943 return conv != (iconv_t) -1; 944 }''', args: config_host['GLIB_CFLAGS'].split() + config_host['GLIB_LIBS'].split() + link_args) 945 iconv = declare_dependency(link_args: link_args, dependencies: glib) 946 break 947 endif 948 endforeach 949 endif 950 if curses.found() and not iconv.found() 951 if get_option('iconv').enabled() 952 error('iconv not available') 953 endif 954 msg = 'iconv required for curses UI but not available' 955 curses = not_found 956 endif 957 if not curses.found() and msg != '' 958 if get_option('curses').enabled() 959 error(msg) 960 else 961 warning(msg + ', disabling') 962 endif 963 endif 964endif 965 966brlapi = not_found 967if not get_option('brlapi').auto() or have_system 968 brlapi = cc.find_library('brlapi', has_headers: ['brlapi.h'], 969 required: get_option('brlapi'), 970 kwargs: static_kwargs) 971 if brlapi.found() and not cc.links(''' 972 #include <brlapi.h> 973 #include <stddef.h> 974 int main(void) { return brlapi__openConnection (NULL, NULL, NULL); }''', dependencies: brlapi) 975 brlapi = not_found 976 if get_option('brlapi').enabled() 977 error('could not link brlapi') 978 else 979 warning('could not link brlapi, disabling') 980 endif 981 endif 982endif 983 984sdl = not_found 985if not get_option('sdl').auto() or have_system 986 sdl = dependency('sdl2', required: get_option('sdl'), kwargs: static_kwargs) 987 sdl_image = not_found 988endif 989if sdl.found() 990 # work around 2.0.8 bug 991 sdl = declare_dependency(compile_args: '-Wno-undef', 992 dependencies: sdl) 993 sdl_image = dependency('SDL2_image', required: get_option('sdl_image'), 994 method: 'pkg-config', kwargs: static_kwargs) 995else 996 if get_option('sdl_image').enabled() 997 error('sdl-image required, but SDL was @0@'.format( 998 get_option('sdl').disabled() ? 'disabled' : 'not found')) 999 endif 1000 sdl_image = not_found 1001endif 1002 1003rbd = not_found 1004if not get_option('rbd').auto() or have_block 1005 librados = cc.find_library('rados', required: get_option('rbd'), 1006 kwargs: static_kwargs) 1007 librbd = cc.find_library('rbd', has_headers: ['rbd/librbd.h'], 1008 required: get_option('rbd'), 1009 kwargs: static_kwargs) 1010 if librados.found() and librbd.found() 1011 if cc.links(''' 1012 #include <stdio.h> 1013 #include <rbd/librbd.h> 1014 int main(void) { 1015 rados_t cluster; 1016 rados_create(&cluster, NULL); 1017 #if LIBRBD_VERSION_CODE < LIBRBD_VERSION(1, 12, 0) 1018 #error 1019 #endif 1020 return 0; 1021 }''', dependencies: [librbd, librados]) 1022 rbd = declare_dependency(dependencies: [librbd, librados]) 1023 elif get_option('rbd').enabled() 1024 error('librbd >= 1.12.0 required') 1025 else 1026 warning('librbd >= 1.12.0 not found, disabling') 1027 endif 1028 endif 1029endif 1030 1031glusterfs = not_found 1032glusterfs_ftruncate_has_stat = false 1033glusterfs_iocb_has_stat = false 1034if not get_option('glusterfs').auto() or have_block 1035 glusterfs = dependency('glusterfs-api', version: '>=3', 1036 required: get_option('glusterfs'), 1037 method: 'pkg-config', kwargs: static_kwargs) 1038 if glusterfs.found() 1039 glusterfs_ftruncate_has_stat = cc.links(''' 1040 #include <glusterfs/api/glfs.h> 1041 1042 int 1043 main(void) 1044 { 1045 /* new glfs_ftruncate() passes two additional args */ 1046 return glfs_ftruncate(NULL, 0, NULL, NULL); 1047 } 1048 ''', dependencies: glusterfs) 1049 glusterfs_iocb_has_stat = cc.links(''' 1050 #include <glusterfs/api/glfs.h> 1051 1052 /* new glfs_io_cbk() passes two additional glfs_stat structs */ 1053 static void 1054 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data) 1055 {} 1056 1057 int 1058 main(void) 1059 { 1060 glfs_io_cbk iocb = &glusterfs_iocb; 1061 iocb(NULL, 0 , NULL, NULL, NULL); 1062 return 0; 1063 } 1064 ''', dependencies: glusterfs) 1065 endif 1066endif 1067 1068libssh = not_found 1069if not get_option('libssh').auto() or have_block 1070 libssh = dependency('libssh', version: '>=0.8.7', 1071 method: 'pkg-config', 1072 required: get_option('libssh'), 1073 kwargs: static_kwargs) 1074endif 1075 1076libbzip2 = not_found 1077if not get_option('bzip2').auto() or have_block 1078 libbzip2 = cc.find_library('bz2', has_headers: ['bzlib.h'], 1079 required: get_option('bzip2'), 1080 kwargs: static_kwargs) 1081 if libbzip2.found() and not cc.links(''' 1082 #include <bzlib.h> 1083 int main(void) { BZ2_bzlibVersion(); return 0; }''', dependencies: libbzip2) 1084 libbzip2 = not_found 1085 if get_option('bzip2').enabled() 1086 error('could not link libbzip2') 1087 else 1088 warning('could not link libbzip2, disabling') 1089 endif 1090 endif 1091endif 1092 1093liblzfse = not_found 1094if not get_option('lzfse').auto() or have_block 1095 liblzfse = cc.find_library('lzfse', has_headers: ['lzfse.h'], 1096 required: get_option('lzfse'), 1097 kwargs: static_kwargs) 1098endif 1099if liblzfse.found() and not cc.links(''' 1100 #include <lzfse.h> 1101 int main(void) { lzfse_decode_scratch_size(); return 0; }''', dependencies: liblzfse) 1102 liblzfse = not_found 1103 if get_option('lzfse').enabled() 1104 error('could not link liblzfse') 1105 else 1106 warning('could not link liblzfse, disabling') 1107 endif 1108endif 1109 1110oss = not_found 1111if get_option('oss').allowed() and have_system 1112 if not cc.has_header('sys/soundcard.h') 1113 # not found 1114 elif targetos == 'netbsd' 1115 oss = cc.find_library('ossaudio', required: get_option('oss'), 1116 kwargs: static_kwargs) 1117 else 1118 oss = declare_dependency() 1119 endif 1120 1121 if not oss.found() 1122 if get_option('oss').enabled() 1123 error('OSS not found') 1124 endif 1125 endif 1126endif 1127dsound = not_found 1128if not get_option('dsound').auto() or (targetos == 'windows' and have_system) 1129 if cc.has_header('dsound.h') 1130 dsound = declare_dependency(link_args: ['-lole32', '-ldxguid']) 1131 endif 1132 1133 if not dsound.found() 1134 if get_option('dsound').enabled() 1135 error('DirectSound not found') 1136 endif 1137 endif 1138endif 1139 1140coreaudio = not_found 1141if not get_option('coreaudio').auto() or (targetos == 'darwin' and have_system) 1142 coreaudio = dependency('appleframeworks', modules: 'CoreAudio', 1143 required: get_option('coreaudio')) 1144endif 1145 1146opengl = not_found 1147if not get_option('opengl').auto() or have_system or have_vhost_user_gpu 1148 epoxy = dependency('epoxy', method: 'pkg-config', 1149 required: get_option('opengl'), kwargs: static_kwargs) 1150 if cc.has_header('epoxy/egl.h', dependencies: epoxy) 1151 opengl = epoxy 1152 elif get_option('opengl').enabled() 1153 error('epoxy/egl.h not found') 1154 endif 1155endif 1156gbm = not_found 1157if (have_system or have_tools) and (virgl.found() or opengl.found()) 1158 gbm = dependency('gbm', method: 'pkg-config', required: false, 1159 kwargs: static_kwargs) 1160endif 1161have_vhost_user_gpu = have_vhost_user_gpu and virgl.found() and opengl.found() and gbm.found() 1162 1163gnutls = not_found 1164gnutls_crypto = not_found 1165if get_option('gnutls').enabled() or (get_option('gnutls').auto() and have_system) 1166 # For general TLS support our min gnutls matches 1167 # that implied by our platform support matrix 1168 # 1169 # For the crypto backends, we look for a newer 1170 # gnutls: 1171 # 1172 # Version 3.6.8 is needed to get XTS 1173 # Version 3.6.13 is needed to get PBKDF 1174 # Version 3.6.14 is needed to get HW accelerated XTS 1175 # 1176 # If newer enough gnutls isn't available, we can 1177 # still use a different crypto backend to satisfy 1178 # the platform support requirements 1179 gnutls_crypto = dependency('gnutls', version: '>=3.6.14', 1180 method: 'pkg-config', 1181 required: false, 1182 kwargs: static_kwargs) 1183 if gnutls_crypto.found() 1184 gnutls = gnutls_crypto 1185 else 1186 # Our min version if all we need is TLS 1187 gnutls = dependency('gnutls', version: '>=3.5.18', 1188 method: 'pkg-config', 1189 required: get_option('gnutls'), 1190 kwargs: static_kwargs) 1191 endif 1192endif 1193 1194# We prefer use of gnutls for crypto, unless the options 1195# explicitly asked for nettle or gcrypt. 1196# 1197# If gnutls isn't available for crypto, then we'll prefer 1198# gcrypt over nettle for performance reasons. 1199gcrypt = not_found 1200nettle = not_found 1201hogweed = not_found 1202xts = 'none' 1203 1204if get_option('nettle').enabled() and get_option('gcrypt').enabled() 1205 error('Only one of gcrypt & nettle can be enabled') 1206endif 1207 1208# Explicit nettle/gcrypt request, so ignore gnutls for crypto 1209if get_option('nettle').enabled() or get_option('gcrypt').enabled() 1210 gnutls_crypto = not_found 1211endif 1212 1213if not gnutls_crypto.found() 1214 if (not get_option('gcrypt').auto() or have_system) and not get_option('nettle').enabled() 1215 gcrypt = dependency('libgcrypt', version: '>=1.8', 1216 method: 'config-tool', 1217 required: get_option('gcrypt'), 1218 kwargs: static_kwargs) 1219 # Debian has removed -lgpg-error from libgcrypt-config 1220 # as it "spreads unnecessary dependencies" which in 1221 # turn breaks static builds... 1222 if gcrypt.found() and enable_static 1223 gcrypt = declare_dependency(dependencies: [ 1224 gcrypt, 1225 cc.find_library('gpg-error', required: true, kwargs: static_kwargs)]) 1226 endif 1227 endif 1228 if (not get_option('nettle').auto() or have_system) and not gcrypt.found() 1229 nettle = dependency('nettle', version: '>=3.4', 1230 method: 'pkg-config', 1231 required: get_option('nettle'), 1232 kwargs: static_kwargs) 1233 if nettle.found() and not cc.has_header('nettle/xts.h', dependencies: nettle) 1234 xts = 'private' 1235 endif 1236 endif 1237endif 1238 1239gmp = dependency('gmp', required: false, method: 'pkg-config', kwargs: static_kwargs) 1240if nettle.found() and gmp.found() 1241 hogweed = dependency('hogweed', version: '>=3.4', 1242 method: 'pkg-config', 1243 required: get_option('nettle'), 1244 kwargs: static_kwargs) 1245endif 1246 1247 1248gtk = not_found 1249gtkx11 = not_found 1250vte = not_found 1251have_gtk_clipboard = get_option('gtk_clipboard').enabled() 1252 1253if not get_option('gtk').auto() or have_system 1254 gtk = dependency('gtk+-3.0', version: '>=3.22.0', 1255 method: 'pkg-config', 1256 required: get_option('gtk'), 1257 kwargs: static_kwargs) 1258 if gtk.found() 1259 gtkx11 = dependency('gtk+-x11-3.0', version: '>=3.22.0', 1260 method: 'pkg-config', 1261 required: false, 1262 kwargs: static_kwargs) 1263 gtk = declare_dependency(dependencies: [gtk, gtkx11]) 1264 1265 if not get_option('vte').auto() or have_system 1266 vte = dependency('vte-2.91', 1267 method: 'pkg-config', 1268 required: get_option('vte'), 1269 kwargs: static_kwargs) 1270 endif 1271 elif have_gtk_clipboard 1272 error('GTK clipboard requested, but GTK not found') 1273 endif 1274endif 1275 1276x11 = not_found 1277if gtkx11.found() 1278 x11 = dependency('x11', method: 'pkg-config', required: gtkx11.found(), 1279 kwargs: static_kwargs) 1280endif 1281png = not_found 1282if get_option('png').allowed() and have_system 1283 png = dependency('libpng', version: '>=1.6.34', required: get_option('png'), 1284 method: 'pkg-config', kwargs: static_kwargs) 1285endif 1286vnc = not_found 1287jpeg = not_found 1288sasl = not_found 1289if get_option('vnc').allowed() and have_system 1290 vnc = declare_dependency() # dummy dependency 1291 jpeg = dependency('libjpeg', required: get_option('vnc_jpeg'), 1292 method: 'pkg-config', kwargs: static_kwargs) 1293 sasl = cc.find_library('sasl2', has_headers: ['sasl/sasl.h'], 1294 required: get_option('vnc_sasl'), 1295 kwargs: static_kwargs) 1296 if sasl.found() 1297 sasl = declare_dependency(dependencies: sasl, 1298 compile_args: '-DSTRUCT_IOVEC_DEFINED') 1299 endif 1300endif 1301 1302pam = not_found 1303if not get_option('auth_pam').auto() or have_system 1304 pam = cc.find_library('pam', has_headers: ['security/pam_appl.h'], 1305 required: get_option('auth_pam'), 1306 kwargs: static_kwargs) 1307endif 1308if pam.found() and not cc.links(''' 1309 #include <stddef.h> 1310 #include <security/pam_appl.h> 1311 int main(void) { 1312 const char *service_name = "qemu"; 1313 const char *user = "frank"; 1314 const struct pam_conv pam_conv = { 0 }; 1315 pam_handle_t *pamh = NULL; 1316 pam_start(service_name, user, &pam_conv, &pamh); 1317 return 0; 1318 }''', dependencies: pam) 1319 pam = not_found 1320 if get_option('auth_pam').enabled() 1321 error('could not link libpam') 1322 else 1323 warning('could not link libpam, disabling') 1324 endif 1325endif 1326 1327snappy = not_found 1328if not get_option('snappy').auto() or have_system 1329 snappy = cc.find_library('snappy', has_headers: ['snappy-c.h'], 1330 required: get_option('snappy'), 1331 kwargs: static_kwargs) 1332endif 1333if snappy.found() and not linker.links(''' 1334 #include <snappy-c.h> 1335 int main(void) { snappy_max_compressed_length(4096); return 0; }''', dependencies: snappy) 1336 snappy = not_found 1337 if get_option('snappy').enabled() 1338 error('could not link libsnappy') 1339 else 1340 warning('could not link libsnappy, disabling') 1341 endif 1342endif 1343 1344lzo = not_found 1345if not get_option('lzo').auto() or have_system 1346 lzo = cc.find_library('lzo2', has_headers: ['lzo/lzo1x.h'], 1347 required: get_option('lzo'), 1348 kwargs: static_kwargs) 1349endif 1350if lzo.found() and not cc.links(''' 1351 #include <lzo/lzo1x.h> 1352 int main(void) { lzo_version(); return 0; }''', dependencies: lzo) 1353 lzo = not_found 1354 if get_option('lzo').enabled() 1355 error('could not link liblzo2') 1356 else 1357 warning('could not link liblzo2, disabling') 1358 endif 1359endif 1360 1361numa = not_found 1362if not get_option('numa').auto() or have_system or have_tools 1363 numa = cc.find_library('numa', has_headers: ['numa.h'], 1364 required: get_option('numa'), 1365 kwargs: static_kwargs) 1366endif 1367if numa.found() and not cc.links(''' 1368 #include <numa.h> 1369 int main(void) { return numa_available(); } 1370 ''', dependencies: numa) 1371 numa = not_found 1372 if get_option('numa').enabled() 1373 error('could not link numa') 1374 else 1375 warning('could not link numa, disabling') 1376 endif 1377endif 1378 1379rdma = not_found 1380if not get_option('rdma').auto() or have_system 1381 libumad = cc.find_library('ibumad', required: get_option('rdma')) 1382 rdma_libs = [cc.find_library('rdmacm', has_headers: ['rdma/rdma_cma.h'], 1383 required: get_option('rdma'), 1384 kwargs: static_kwargs), 1385 cc.find_library('ibverbs', required: get_option('rdma'), 1386 kwargs: static_kwargs), 1387 libumad] 1388 rdma = declare_dependency(dependencies: rdma_libs) 1389 foreach lib: rdma_libs 1390 if not lib.found() 1391 rdma = not_found 1392 endif 1393 endforeach 1394endif 1395 1396xen = not_found 1397if get_option('xen').enabled() or (get_option('xen').auto() and have_system) 1398 xencontrol = dependency('xencontrol', required: false, 1399 method: 'pkg-config', kwargs: static_kwargs) 1400 if xencontrol.found() 1401 xen_pc = declare_dependency(version: xencontrol.version(), 1402 dependencies: [ 1403 xencontrol, 1404 # disabler: true makes xen_pc.found() return false if any is not found 1405 dependency('xenstore', required: false, 1406 method: 'pkg-config', kwargs: static_kwargs, 1407 disabler: true), 1408 dependency('xenforeignmemory', required: false, 1409 method: 'pkg-config', kwargs: static_kwargs, 1410 disabler: true), 1411 dependency('xengnttab', required: false, 1412 method: 'pkg-config', kwargs: static_kwargs, 1413 disabler: true), 1414 dependency('xenevtchn', required: false, 1415 method: 'pkg-config', kwargs: static_kwargs, 1416 disabler: true), 1417 dependency('xendevicemodel', required: false, 1418 method: 'pkg-config', kwargs: static_kwargs, 1419 disabler: true), 1420 # optional, no "disabler: true" 1421 dependency('xentoolcore', required: false, 1422 method: 'pkg-config', kwargs: static_kwargs)]) 1423 if xen_pc.found() 1424 xen = xen_pc 1425 endif 1426 endif 1427 if not xen.found() 1428 xen_tests = [ '4.11.0', '4.10.0', '4.9.0', '4.8.0', '4.7.1', '4.6.0', '4.5.0', '4.2.0' ] 1429 xen_libs = { 1430 '4.11.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ], 1431 '4.10.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn', 'xentoolcore' ], 1432 '4.9.0': [ 'xenstore', 'xenctrl', 'xendevicemodel', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ], 1433 '4.8.0': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ], 1434 '4.7.1': [ 'xenstore', 'xenctrl', 'xenforeignmemory', 'xengnttab', 'xenevtchn' ], 1435 '4.6.0': [ 'xenstore', 'xenctrl' ], 1436 '4.5.0': [ 'xenstore', 'xenctrl' ], 1437 '4.2.0': [ 'xenstore', 'xenctrl' ], 1438 } 1439 xen_deps = {} 1440 foreach ver: xen_tests 1441 # cache the various library tests to avoid polluting the logs 1442 xen_test_deps = [] 1443 foreach l: xen_libs[ver] 1444 if l not in xen_deps 1445 xen_deps += { l: cc.find_library(l, required: false) } 1446 endif 1447 xen_test_deps += xen_deps[l] 1448 endforeach 1449 1450 # Use -D to pick just one of the test programs in scripts/xen-detect.c 1451 xen_version = ver.split('.') 1452 xen_ctrl_version = xen_version[0] + \ 1453 ('0' + xen_version[1]).substring(-2) + \ 1454 ('0' + xen_version[2]).substring(-2) 1455 if cc.links(files('scripts/xen-detect.c'), 1456 args: '-DCONFIG_XEN_CTRL_INTERFACE_VERSION=' + xen_ctrl_version, 1457 dependencies: xen_test_deps) 1458 xen = declare_dependency(version: ver, dependencies: xen_test_deps) 1459 break 1460 endif 1461 endforeach 1462 endif 1463 if xen.found() 1464 accelerators += 'CONFIG_XEN' 1465 elif get_option('xen').enabled() 1466 error('could not compile and link Xen test program') 1467 endif 1468endif 1469have_xen_pci_passthrough = get_option('xen_pci_passthrough') \ 1470 .require(xen.found(), 1471 error_message: 'Xen PCI passthrough requested but Xen not enabled') \ 1472 .require(targetos == 'linux', 1473 error_message: 'Xen PCI passthrough not available on this platform') \ 1474 .allowed() 1475 1476 1477cacard = not_found 1478if not get_option('smartcard').auto() or have_system 1479 cacard = dependency('libcacard', required: get_option('smartcard'), 1480 version: '>=2.5.1', method: 'pkg-config', 1481 kwargs: static_kwargs) 1482endif 1483u2f = not_found 1484if have_system 1485 u2f = dependency('u2f-emu', required: get_option('u2f'), 1486 method: 'pkg-config', 1487 kwargs: static_kwargs) 1488endif 1489canokey = not_found 1490if have_system 1491 canokey = dependency('canokey-qemu', required: get_option('canokey'), 1492 method: 'pkg-config', 1493 kwargs: static_kwargs) 1494endif 1495usbredir = not_found 1496if not get_option('usb_redir').auto() or have_system 1497 usbredir = dependency('libusbredirparser-0.5', required: get_option('usb_redir'), 1498 version: '>=0.6', method: 'pkg-config', 1499 kwargs: static_kwargs) 1500endif 1501libusb = not_found 1502if not get_option('libusb').auto() or have_system 1503 libusb = dependency('libusb-1.0', required: get_option('libusb'), 1504 version: '>=1.0.13', method: 'pkg-config', 1505 kwargs: static_kwargs) 1506endif 1507 1508libpmem = not_found 1509if not get_option('libpmem').auto() or have_system 1510 libpmem = dependency('libpmem', required: get_option('libpmem'), 1511 method: 'pkg-config', kwargs: static_kwargs) 1512endif 1513libdaxctl = not_found 1514if not get_option('libdaxctl').auto() or have_system 1515 libdaxctl = dependency('libdaxctl', required: get_option('libdaxctl'), 1516 version: '>=57', method: 'pkg-config', 1517 kwargs: static_kwargs) 1518endif 1519tasn1 = not_found 1520if gnutls.found() 1521 tasn1 = dependency('libtasn1', 1522 method: 'pkg-config', 1523 kwargs: static_kwargs) 1524endif 1525keyutils = dependency('libkeyutils', required: false, 1526 method: 'pkg-config', kwargs: static_kwargs) 1527 1528has_gettid = cc.has_function('gettid') 1529 1530# libselinux 1531selinux = dependency('libselinux', 1532 required: get_option('selinux'), 1533 method: 'pkg-config', kwargs: static_kwargs) 1534 1535# Malloc tests 1536 1537malloc = [] 1538if get_option('malloc') == 'system' 1539 has_malloc_trim = \ 1540 get_option('malloc_trim').allowed() and \ 1541 cc.links('''#include <malloc.h> 1542 int main(void) { malloc_trim(0); return 0; }''') 1543else 1544 has_malloc_trim = false 1545 malloc = cc.find_library(get_option('malloc'), required: true) 1546endif 1547if not has_malloc_trim and get_option('malloc_trim').enabled() 1548 if get_option('malloc') == 'system' 1549 error('malloc_trim not available on this platform.') 1550 else 1551 error('malloc_trim not available with non-libc memory allocator') 1552 endif 1553endif 1554 1555# Check whether the glibc provides statx() 1556 1557gnu_source_prefix = ''' 1558 #ifndef _GNU_SOURCE 1559 #define _GNU_SOURCE 1560 #endif 1561''' 1562statx_test = gnu_source_prefix + ''' 1563 #include <sys/stat.h> 1564 int main(void) { 1565 struct statx statxbuf; 1566 statx(0, "", 0, STATX_BASIC_STATS, &statxbuf); 1567 return 0; 1568 }''' 1569 1570has_statx = cc.links(statx_test) 1571 1572# Check whether statx() provides mount ID information 1573 1574statx_mnt_id_test = gnu_source_prefix + ''' 1575 #include <sys/stat.h> 1576 int main(void) { 1577 struct statx statxbuf; 1578 statx(0, "", 0, STATX_BASIC_STATS | STATX_MNT_ID, &statxbuf); 1579 return statxbuf.stx_mnt_id; 1580 }''' 1581 1582has_statx_mnt_id = cc.links(statx_mnt_id_test) 1583 1584have_vhost_user_blk_server = get_option('vhost_user_blk_server') \ 1585 .require(targetos == 'linux', 1586 error_message: 'vhost_user_blk_server requires linux') \ 1587 .require(have_vhost_user, 1588 error_message: 'vhost_user_blk_server requires vhost-user support') \ 1589 .disable_auto_if(not have_tools and not have_system) \ 1590 .allowed() 1591 1592if get_option('fuse').disabled() and get_option('fuse_lseek').enabled() 1593 error('Cannot enable fuse-lseek while fuse is disabled') 1594endif 1595 1596fuse = dependency('fuse3', required: get_option('fuse'), 1597 version: '>=3.1', method: 'pkg-config', 1598 kwargs: static_kwargs) 1599 1600fuse_lseek = not_found 1601if get_option('fuse_lseek').allowed() 1602 if fuse.version().version_compare('>=3.8') 1603 # Dummy dependency 1604 fuse_lseek = declare_dependency() 1605 elif get_option('fuse_lseek').enabled() 1606 if fuse.found() 1607 error('fuse-lseek requires libfuse >=3.8, found ' + fuse.version()) 1608 else 1609 error('fuse-lseek requires libfuse, which was not found') 1610 endif 1611 endif 1612endif 1613 1614have_libvduse = (targetos == 'linux') 1615if get_option('libvduse').enabled() 1616 if targetos != 'linux' 1617 error('libvduse requires linux') 1618 endif 1619elif get_option('libvduse').disabled() 1620 have_libvduse = false 1621endif 1622 1623have_vduse_blk_export = (have_libvduse and targetos == 'linux') 1624if get_option('vduse_blk_export').enabled() 1625 if targetos != 'linux' 1626 error('vduse_blk_export requires linux') 1627 elif not have_libvduse 1628 error('vduse_blk_export requires libvduse support') 1629 endif 1630elif get_option('vduse_blk_export').disabled() 1631 have_vduse_blk_export = false 1632endif 1633 1634# libbpf 1635libbpf = dependency('libbpf', required: get_option('bpf'), method: 'pkg-config') 1636if libbpf.found() and not cc.links(''' 1637 #include <bpf/libbpf.h> 1638 int main(void) 1639 { 1640 bpf_object__destroy_skeleton(NULL); 1641 return 0; 1642 }''', dependencies: libbpf) 1643 libbpf = not_found 1644 if get_option('bpf').enabled() 1645 error('libbpf skeleton test failed') 1646 else 1647 warning('libbpf skeleton test failed, disabling') 1648 endif 1649endif 1650 1651# libdw 1652libdw = not_found 1653if not get_option('libdw').auto() or \ 1654 (not enable_static and (have_system or have_user)) 1655 libdw = dependency('libdw', 1656 method: 'pkg-config', 1657 kwargs: static_kwargs, 1658 required: get_option('libdw')) 1659endif 1660 1661################# 1662# config-host.h # 1663################# 1664 1665audio_drivers_selected = [] 1666if have_system 1667 audio_drivers_available = { 1668 'alsa': alsa.found(), 1669 'coreaudio': coreaudio.found(), 1670 'dsound': dsound.found(), 1671 'jack': jack.found(), 1672 'oss': oss.found(), 1673 'pa': pulse.found(), 1674 'sdl': sdl.found(), 1675 'sndio': sndio.found(), 1676 } 1677 foreach k, v: audio_drivers_available 1678 config_host_data.set('CONFIG_AUDIO_' + k.to_upper(), v) 1679 endforeach 1680 1681 # Default to native drivers first, OSS second, SDL third 1682 audio_drivers_priority = \ 1683 [ 'pa', 'coreaudio', 'dsound', 'sndio', 'oss' ] + \ 1684 (targetos == 'linux' ? [] : [ 'sdl' ]) 1685 audio_drivers_default = [] 1686 foreach k: audio_drivers_priority 1687 if audio_drivers_available[k] 1688 audio_drivers_default += k 1689 endif 1690 endforeach 1691 1692 foreach k: get_option('audio_drv_list') 1693 if k == 'default' 1694 audio_drivers_selected += audio_drivers_default 1695 elif not audio_drivers_available[k] 1696 error('Audio driver "@0@" not available.'.format(k)) 1697 else 1698 audio_drivers_selected += k 1699 endif 1700 endforeach 1701endif 1702config_host_data.set('CONFIG_AUDIO_DRIVERS', 1703 '"' + '", "'.join(audio_drivers_selected) + '", ') 1704 1705if get_option('cfi') 1706 cfi_flags=[] 1707 # Check for dependency on LTO 1708 if not get_option('b_lto') 1709 error('Selected Control-Flow Integrity but LTO is disabled') 1710 endif 1711 if config_host.has_key('CONFIG_MODULES') 1712 error('Selected Control-Flow Integrity is not compatible with modules') 1713 endif 1714 # Check for cfi flags. CFI requires LTO so we can't use 1715 # get_supported_arguments, but need a more complex "compiles" which allows 1716 # custom arguments 1717 if cc.compiles('int main () { return 0; }', name: '-fsanitize=cfi-icall', 1718 args: ['-flto', '-fsanitize=cfi-icall'] ) 1719 cfi_flags += '-fsanitize=cfi-icall' 1720 else 1721 error('-fsanitize=cfi-icall is not supported by the compiler') 1722 endif 1723 if cc.compiles('int main () { return 0; }', 1724 name: '-fsanitize-cfi-icall-generalize-pointers', 1725 args: ['-flto', '-fsanitize=cfi-icall', 1726 '-fsanitize-cfi-icall-generalize-pointers'] ) 1727 cfi_flags += '-fsanitize-cfi-icall-generalize-pointers' 1728 else 1729 error('-fsanitize-cfi-icall-generalize-pointers is not supported by the compiler') 1730 endif 1731 if get_option('cfi_debug') 1732 if cc.compiles('int main () { return 0; }', 1733 name: '-fno-sanitize-trap=cfi-icall', 1734 args: ['-flto', '-fsanitize=cfi-icall', 1735 '-fno-sanitize-trap=cfi-icall'] ) 1736 cfi_flags += '-fno-sanitize-trap=cfi-icall' 1737 else 1738 error('-fno-sanitize-trap=cfi-icall is not supported by the compiler') 1739 endif 1740 endif 1741 add_global_arguments(cfi_flags, native: false, language: all_languages) 1742 add_global_link_arguments(cfi_flags, native: false, language: all_languages) 1743endif 1744 1745have_host_block_device = (targetos != 'darwin' or 1746 cc.has_header('IOKit/storage/IOMedia.h')) 1747 1748dbus_display = get_option('dbus_display') \ 1749 .require(gio.version().version_compare('>=2.64'), 1750 error_message: '-display dbus requires glib>=2.64') \ 1751 .require(gdbus_codegen.found(), 1752 error_message: gdbus_codegen_error.format('-display dbus')) \ 1753 .require(opengl.found() and gbm.found(), 1754 error_message: '-display dbus requires epoxy/egl and gbm') \ 1755 .allowed() 1756 1757have_virtfs = get_option('virtfs') \ 1758 .require(targetos == 'linux' or targetos == 'darwin', 1759 error_message: 'virtio-9p (virtfs) requires Linux or macOS') \ 1760 .require(targetos == 'linux' or cc.has_function('pthread_fchdir_np'), 1761 error_message: 'virtio-9p (virtfs) on macOS requires the presence of pthread_fchdir_np') \ 1762 .require(targetos == 'darwin' or (libattr.found() and libcap_ng.found()), 1763 error_message: 'virtio-9p (virtfs) on Linux requires libcap-ng-devel and libattr-devel') \ 1764 .disable_auto_if(not have_tools and not have_system) \ 1765 .allowed() 1766 1767have_virtfs_proxy_helper = targetos != 'darwin' and have_virtfs and have_tools 1768 1769if get_option('block_drv_ro_whitelist') == '' 1770 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', '') 1771else 1772 config_host_data.set('CONFIG_BDRV_RO_WHITELIST', 1773 '"' + get_option('block_drv_ro_whitelist').replace(',', '", "') + '", ') 1774endif 1775if get_option('block_drv_rw_whitelist') == '' 1776 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', '') 1777else 1778 config_host_data.set('CONFIG_BDRV_RW_WHITELIST', 1779 '"' + get_option('block_drv_rw_whitelist').replace(',', '", "') + '", ') 1780endif 1781 1782foreach k : get_option('trace_backends') 1783 config_host_data.set('CONFIG_TRACE_' + k.to_upper(), true) 1784endforeach 1785config_host_data.set_quoted('CONFIG_TRACE_FILE', get_option('trace_file')) 1786config_host_data.set_quoted('CONFIG_TLS_PRIORITY', get_option('tls_priority')) 1787if iasl.found() 1788 config_host_data.set_quoted('CONFIG_IASL', iasl.full_path()) 1789endif 1790config_host_data.set_quoted('CONFIG_BINDIR', get_option('prefix') / get_option('bindir')) 1791config_host_data.set_quoted('CONFIG_PREFIX', get_option('prefix')) 1792config_host_data.set_quoted('CONFIG_QEMU_CONFDIR', get_option('prefix') / qemu_confdir) 1793config_host_data.set_quoted('CONFIG_QEMU_DATADIR', get_option('prefix') / qemu_datadir) 1794config_host_data.set_quoted('CONFIG_QEMU_DESKTOPDIR', get_option('prefix') / qemu_desktopdir) 1795 1796qemu_firmwarepath = '' 1797foreach k : get_option('qemu_firmwarepath') 1798 qemu_firmwarepath += '"' + get_option('prefix') / k + '", ' 1799endforeach 1800config_host_data.set('CONFIG_QEMU_FIRMWAREPATH', qemu_firmwarepath) 1801 1802config_host_data.set_quoted('CONFIG_QEMU_HELPERDIR', get_option('prefix') / get_option('libexecdir')) 1803config_host_data.set_quoted('CONFIG_QEMU_ICONDIR', get_option('prefix') / qemu_icondir) 1804config_host_data.set_quoted('CONFIG_QEMU_LOCALEDIR', get_option('prefix') / get_option('localedir')) 1805config_host_data.set_quoted('CONFIG_QEMU_LOCALSTATEDIR', get_option('prefix') / get_option('localstatedir')) 1806config_host_data.set_quoted('CONFIG_QEMU_MODDIR', get_option('prefix') / qemu_moddir) 1807config_host_data.set_quoted('CONFIG_SYSCONFDIR', get_option('prefix') / get_option('sysconfdir')) 1808 1809if config_host.has_key('CONFIG_MODULES') 1810 config_host_data.set('CONFIG_STAMP', run_command( 1811 meson.current_source_dir() / 'scripts/qemu-stamp.py', 1812 meson.project_version(), get_option('pkgversion'), '--', 1813 meson.current_source_dir() / 'configure', 1814 capture: true, check: true).stdout().strip()) 1815endif 1816 1817have_slirp_smbd = get_option('slirp_smbd') \ 1818 .require(targetos != 'windows', error_message: 'Host smbd not supported on this platform.') \ 1819 .allowed() 1820if have_slirp_smbd 1821 smbd_path = get_option('smbd') 1822 if smbd_path == '' 1823 smbd_path = (targetos == 'solaris' ? '/usr/sfw/sbin/smbd' : '/usr/sbin/smbd') 1824 endif 1825 config_host_data.set_quoted('CONFIG_SMBD_COMMAND', smbd_path) 1826endif 1827 1828config_host_data.set('HOST_' + host_arch.to_upper(), 1) 1829 1830if get_option('module_upgrades') and not enable_modules 1831 error('Cannot enable module-upgrades as modules are not enabled') 1832endif 1833config_host_data.set('CONFIG_MODULE_UPGRADES', get_option('module_upgrades')) 1834 1835config_host_data.set('CONFIG_ATTR', libattr.found()) 1836config_host_data.set('CONFIG_BDRV_WHITELIST_TOOLS', get_option('block_drv_whitelist_in_tools')) 1837config_host_data.set('CONFIG_BRLAPI', brlapi.found()) 1838config_host_data.set('CONFIG_COCOA', cocoa.found()) 1839config_host_data.set('CONFIG_FUZZ', get_option('fuzzing')) 1840config_host_data.set('CONFIG_GCOV', get_option('b_coverage')) 1841config_host_data.set('CONFIG_LIBUDEV', libudev.found()) 1842config_host_data.set('CONFIG_LZO', lzo.found()) 1843config_host_data.set('CONFIG_MPATH', mpathpersist.found()) 1844config_host_data.set('CONFIG_MPATH_NEW_API', mpathpersist_new_api) 1845config_host_data.set('CONFIG_BLKIO', blkio.found()) 1846config_host_data.set('CONFIG_CURL', curl.found()) 1847config_host_data.set('CONFIG_CURSES', curses.found()) 1848config_host_data.set('CONFIG_GBM', gbm.found()) 1849config_host_data.set('CONFIG_GIO', gio.found()) 1850config_host_data.set('CONFIG_GLUSTERFS', glusterfs.found()) 1851if glusterfs.found() 1852 config_host_data.set('CONFIG_GLUSTERFS_XLATOR_OPT', glusterfs.version().version_compare('>=4')) 1853 config_host_data.set('CONFIG_GLUSTERFS_DISCARD', glusterfs.version().version_compare('>=5')) 1854 config_host_data.set('CONFIG_GLUSTERFS_FALLOCATE', glusterfs.version().version_compare('>=6')) 1855 config_host_data.set('CONFIG_GLUSTERFS_ZEROFILL', glusterfs.version().version_compare('>=6')) 1856 config_host_data.set('CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT', glusterfs_ftruncate_has_stat) 1857 config_host_data.set('CONFIG_GLUSTERFS_IOCB_HAS_STAT', glusterfs_iocb_has_stat) 1858endif 1859config_host_data.set('CONFIG_GTK', gtk.found()) 1860config_host_data.set('CONFIG_VTE', vte.found()) 1861config_host_data.set('CONFIG_GTK_CLIPBOARD', have_gtk_clipboard) 1862config_host_data.set('CONFIG_LIBATTR', have_old_libattr) 1863config_host_data.set('CONFIG_LIBCAP_NG', libcap_ng.found()) 1864config_host_data.set('CONFIG_EBPF', libbpf.found()) 1865config_host_data.set('CONFIG_LIBDAXCTL', libdaxctl.found()) 1866config_host_data.set('CONFIG_LIBISCSI', libiscsi.found()) 1867config_host_data.set('CONFIG_LIBNFS', libnfs.found()) 1868config_host_data.set('CONFIG_LIBSSH', libssh.found()) 1869config_host_data.set('CONFIG_LINUX_AIO', libaio.found()) 1870config_host_data.set('CONFIG_LINUX_IO_URING', linux_io_uring.found()) 1871config_host_data.set('CONFIG_LIBPMEM', libpmem.found()) 1872config_host_data.set('CONFIG_NUMA', numa.found()) 1873if numa.found() 1874 config_host_data.set('HAVE_NUMA_HAS_PREFERRED_MANY', 1875 cc.has_function('numa_has_preferred_many', 1876 dependencies: numa)) 1877endif 1878config_host_data.set('CONFIG_OPENGL', opengl.found()) 1879config_host_data.set('CONFIG_PROFILER', get_option('profiler')) 1880config_host_data.set('CONFIG_RBD', rbd.found()) 1881config_host_data.set('CONFIG_RDMA', rdma.found()) 1882config_host_data.set('CONFIG_SDL', sdl.found()) 1883config_host_data.set('CONFIG_SDL_IMAGE', sdl_image.found()) 1884config_host_data.set('CONFIG_SECCOMP', seccomp.found()) 1885if seccomp.found() 1886 config_host_data.set('CONFIG_SECCOMP_SYSRAWRC', seccomp_has_sysrawrc) 1887endif 1888config_host_data.set('CONFIG_SNAPPY', snappy.found()) 1889config_host_data.set('CONFIG_TPM', have_tpm) 1890config_host_data.set('CONFIG_USB_LIBUSB', libusb.found()) 1891config_host_data.set('CONFIG_VDE', vde.found()) 1892config_host_data.set('CONFIG_VHOST_NET', have_vhost_net) 1893config_host_data.set('CONFIG_VHOST_NET_USER', have_vhost_net_user) 1894config_host_data.set('CONFIG_VHOST_NET_VDPA', have_vhost_net_vdpa) 1895config_host_data.set('CONFIG_VHOST_KERNEL', have_vhost_kernel) 1896config_host_data.set('CONFIG_VHOST_USER', have_vhost_user) 1897config_host_data.set('CONFIG_VHOST_CRYPTO', have_vhost_user_crypto) 1898config_host_data.set('CONFIG_VHOST_VDPA', have_vhost_vdpa) 1899config_host_data.set('CONFIG_VMNET', vmnet.found()) 1900config_host_data.set('CONFIG_VHOST_USER_BLK_SERVER', have_vhost_user_blk_server) 1901config_host_data.set('CONFIG_VDUSE_BLK_EXPORT', have_vduse_blk_export) 1902config_host_data.set('CONFIG_PNG', png.found()) 1903config_host_data.set('CONFIG_VNC', vnc.found()) 1904config_host_data.set('CONFIG_VNC_JPEG', jpeg.found()) 1905config_host_data.set('CONFIG_VNC_SASL', sasl.found()) 1906config_host_data.set('CONFIG_VIRTFS', have_virtfs) 1907config_host_data.set('CONFIG_VTE', vte.found()) 1908config_host_data.set('CONFIG_XKBCOMMON', xkbcommon.found()) 1909config_host_data.set('CONFIG_KEYUTILS', keyutils.found()) 1910config_host_data.set('CONFIG_GETTID', has_gettid) 1911config_host_data.set('CONFIG_GNUTLS', gnutls.found()) 1912config_host_data.set('CONFIG_GNUTLS_CRYPTO', gnutls_crypto.found()) 1913config_host_data.set('CONFIG_TASN1', tasn1.found()) 1914config_host_data.set('CONFIG_GCRYPT', gcrypt.found()) 1915config_host_data.set('CONFIG_NETTLE', nettle.found()) 1916config_host_data.set('CONFIG_HOGWEED', hogweed.found()) 1917config_host_data.set('CONFIG_QEMU_PRIVATE_XTS', xts == 'private') 1918config_host_data.set('CONFIG_MALLOC_TRIM', has_malloc_trim) 1919config_host_data.set('CONFIG_STATX', has_statx) 1920config_host_data.set('CONFIG_STATX_MNT_ID', has_statx_mnt_id) 1921config_host_data.set('CONFIG_ZSTD', zstd.found()) 1922config_host_data.set('CONFIG_FUSE', fuse.found()) 1923config_host_data.set('CONFIG_FUSE_LSEEK', fuse_lseek.found()) 1924config_host_data.set('CONFIG_SPICE_PROTOCOL', spice_protocol.found()) 1925if spice_protocol.found() 1926config_host_data.set('CONFIG_SPICE_PROTOCOL_MAJOR', spice_protocol.version().split('.')[0]) 1927config_host_data.set('CONFIG_SPICE_PROTOCOL_MINOR', spice_protocol.version().split('.')[1]) 1928config_host_data.set('CONFIG_SPICE_PROTOCOL_MICRO', spice_protocol.version().split('.')[2]) 1929endif 1930config_host_data.set('CONFIG_SPICE', spice.found()) 1931config_host_data.set('CONFIG_X11', x11.found()) 1932config_host_data.set('CONFIG_DBUS_DISPLAY', dbus_display) 1933config_host_data.set('CONFIG_CFI', get_option('cfi')) 1934config_host_data.set('CONFIG_SELINUX', selinux.found()) 1935config_host_data.set('CONFIG_XEN_BACKEND', xen.found()) 1936config_host_data.set('CONFIG_LIBDW', libdw.found()) 1937if xen.found() 1938 # protect from xen.version() having less than three components 1939 xen_version = xen.version().split('.') + ['0', '0'] 1940 xen_ctrl_version = xen_version[0] + \ 1941 ('0' + xen_version[1]).substring(-2) + \ 1942 ('0' + xen_version[2]).substring(-2) 1943 config_host_data.set('CONFIG_XEN_CTRL_INTERFACE_VERSION', xen_ctrl_version) 1944endif 1945config_host_data.set('QEMU_VERSION', '"@0@"'.format(meson.project_version())) 1946config_host_data.set('QEMU_VERSION_MAJOR', meson.project_version().split('.')[0]) 1947config_host_data.set('QEMU_VERSION_MINOR', meson.project_version().split('.')[1]) 1948config_host_data.set('QEMU_VERSION_MICRO', meson.project_version().split('.')[2]) 1949 1950config_host_data.set_quoted('CONFIG_HOST_DSOSUF', host_dsosuf) 1951config_host_data.set('HAVE_HOST_BLOCK_DEVICE', have_host_block_device) 1952 1953have_coroutine_pool = get_option('coroutine_pool') 1954if get_option('debug_stack_usage') and have_coroutine_pool 1955 message('Disabling coroutine pool to measure stack usage') 1956 have_coroutine_pool = false 1957endif 1958config_host_data.set10('CONFIG_COROUTINE_POOL', have_coroutine_pool) 1959config_host_data.set('CONFIG_DEBUG_MUTEX', get_option('debug_mutex')) 1960config_host_data.set('CONFIG_DEBUG_STACK_USAGE', get_option('debug_stack_usage')) 1961config_host_data.set('CONFIG_GPROF', get_option('gprof')) 1962config_host_data.set('CONFIG_LIVE_BLOCK_MIGRATION', get_option('live_block_migration').allowed()) 1963config_host_data.set('CONFIG_QOM_CAST_DEBUG', get_option('qom_cast_debug')) 1964config_host_data.set('CONFIG_REPLICATION', get_option('replication').allowed()) 1965 1966# has_header 1967config_host_data.set('CONFIG_EPOLL', cc.has_header('sys/epoll.h')) 1968config_host_data.set('CONFIG_LINUX_MAGIC_H', cc.has_header('linux/magic.h')) 1969config_host_data.set('CONFIG_VALGRIND_H', cc.has_header('valgrind/valgrind.h')) 1970config_host_data.set('HAVE_BTRFS_H', cc.has_header('linux/btrfs.h')) 1971config_host_data.set('HAVE_DRM_H', cc.has_header('libdrm/drm.h')) 1972config_host_data.set('HAVE_PTY_H', cc.has_header('pty.h')) 1973config_host_data.set('HAVE_SYS_DISK_H', cc.has_header('sys/disk.h')) 1974config_host_data.set('HAVE_SYS_IOCCOM_H', cc.has_header('sys/ioccom.h')) 1975config_host_data.set('HAVE_SYS_KCOV_H', cc.has_header('sys/kcov.h')) 1976if targetos == 'windows' 1977 config_host_data.set('HAVE_AFUNIX_H', cc.has_header('afunix.h')) 1978endif 1979 1980# has_function 1981config_host_data.set('CONFIG_CLOSE_RANGE', cc.has_function('close_range')) 1982config_host_data.set('CONFIG_ACCEPT4', cc.has_function('accept4')) 1983config_host_data.set('CONFIG_CLOCK_ADJTIME', cc.has_function('clock_adjtime')) 1984config_host_data.set('CONFIG_DUP3', cc.has_function('dup3')) 1985config_host_data.set('CONFIG_FALLOCATE', cc.has_function('fallocate')) 1986config_host_data.set('CONFIG_POSIX_FALLOCATE', cc.has_function('posix_fallocate')) 1987# Note that we need to specify prefix: here to avoid incorrectly 1988# thinking that Windows has posix_memalign() 1989config_host_data.set('CONFIG_POSIX_MEMALIGN', cc.has_function('posix_memalign', prefix: '#include <stdlib.h>')) 1990config_host_data.set('CONFIG_ALIGNED_MALLOC', cc.has_function('_aligned_malloc')) 1991config_host_data.set('CONFIG_VALLOC', cc.has_function('valloc')) 1992config_host_data.set('CONFIG_MEMALIGN', cc.has_function('memalign')) 1993config_host_data.set('CONFIG_PPOLL', cc.has_function('ppoll')) 1994config_host_data.set('CONFIG_PREADV', cc.has_function('preadv', prefix: '#include <sys/uio.h>')) 1995config_host_data.set('CONFIG_PTHREAD_FCHDIR_NP', cc.has_function('pthread_fchdir_np')) 1996config_host_data.set('CONFIG_SENDFILE', cc.has_function('sendfile')) 1997config_host_data.set('CONFIG_SETNS', cc.has_function('setns') and cc.has_function('unshare')) 1998config_host_data.set('CONFIG_SYNCFS', cc.has_function('syncfs')) 1999config_host_data.set('CONFIG_SYNC_FILE_RANGE', cc.has_function('sync_file_range')) 2000config_host_data.set('CONFIG_TIMERFD', cc.has_function('timerfd_create')) 2001config_host_data.set('HAVE_COPY_FILE_RANGE', cc.has_function('copy_file_range')) 2002config_host_data.set('HAVE_GETIFADDRS', cc.has_function('getifaddrs')) 2003config_host_data.set('HAVE_OPENPTY', cc.has_function('openpty', dependencies: util)) 2004config_host_data.set('HAVE_STRCHRNUL', cc.has_function('strchrnul')) 2005config_host_data.set('HAVE_SYSTEM_FUNCTION', cc.has_function('system', prefix: '#include <stdlib.h>')) 2006if rbd.found() 2007 config_host_data.set('HAVE_RBD_NAMESPACE_EXISTS', 2008 cc.has_function('rbd_namespace_exists', 2009 dependencies: rbd, 2010 prefix: '#include <rbd/librbd.h>')) 2011endif 2012if rdma.found() 2013 config_host_data.set('HAVE_IBV_ADVISE_MR', 2014 cc.has_function('ibv_advise_mr', 2015 dependencies: rdma, 2016 prefix: '#include <infiniband/verbs.h>')) 2017endif 2018 2019# has_header_symbol 2020config_host_data.set('CONFIG_EPOLL_CREATE1', 2021 cc.has_header_symbol('sys/epoll.h', 'epoll_create1')) 2022config_host_data.set('CONFIG_FALLOCATE_PUNCH_HOLE', 2023 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_PUNCH_HOLE') and 2024 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_KEEP_SIZE')) 2025config_host_data.set('CONFIG_FALLOCATE_ZERO_RANGE', 2026 cc.has_header_symbol('linux/falloc.h', 'FALLOC_FL_ZERO_RANGE')) 2027config_host_data.set('CONFIG_FIEMAP', 2028 cc.has_header('linux/fiemap.h') and 2029 cc.has_header_symbol('linux/fs.h', 'FS_IOC_FIEMAP')) 2030config_host_data.set('CONFIG_GETRANDOM', 2031 cc.has_function('getrandom') and 2032 cc.has_header_symbol('sys/random.h', 'GRND_NONBLOCK')) 2033config_host_data.set('CONFIG_INOTIFY', 2034 cc.has_header_symbol('sys/inotify.h', 'inotify_init')) 2035config_host_data.set('CONFIG_INOTIFY1', 2036 cc.has_header_symbol('sys/inotify.h', 'inotify_init1')) 2037config_host_data.set('CONFIG_PRCTL_PR_SET_TIMERSLACK', 2038 cc.has_header_symbol('sys/prctl.h', 'PR_SET_TIMERSLACK')) 2039config_host_data.set('CONFIG_RTNETLINK', 2040 cc.has_header_symbol('linux/rtnetlink.h', 'IFLA_PROTO_DOWN')) 2041config_host_data.set('CONFIG_SYSMACROS', 2042 cc.has_header_symbol('sys/sysmacros.h', 'makedev')) 2043config_host_data.set('HAVE_OPTRESET', 2044 cc.has_header_symbol('getopt.h', 'optreset')) 2045config_host_data.set('HAVE_IPPROTO_MPTCP', 2046 cc.has_header_symbol('netinet/in.h', 'IPPROTO_MPTCP')) 2047 2048# has_member 2049config_host_data.set('HAVE_SIGEV_NOTIFY_THREAD_ID', 2050 cc.has_member('struct sigevent', 'sigev_notify_thread_id', 2051 prefix: '#include <signal.h>')) 2052config_host_data.set('HAVE_STRUCT_STAT_ST_ATIM', 2053 cc.has_member('struct stat', 'st_atim', 2054 prefix: '#include <sys/stat.h>')) 2055 2056# has_type 2057config_host_data.set('CONFIG_IOVEC', 2058 cc.has_type('struct iovec', 2059 prefix: '#include <sys/uio.h>')) 2060config_host_data.set('HAVE_UTMPX', 2061 cc.has_type('struct utmpx', 2062 prefix: '#include <utmpx.h>')) 2063 2064config_host_data.set('CONFIG_EVENTFD', cc.links(''' 2065 #include <sys/eventfd.h> 2066 int main(void) { return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC); }''')) 2067config_host_data.set('CONFIG_FDATASYNC', cc.links(gnu_source_prefix + ''' 2068 #include <unistd.h> 2069 int main(void) { 2070 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0 2071 return fdatasync(0); 2072 #else 2073 #error Not supported 2074 #endif 2075 }''')) 2076 2077has_madvise = cc.links(gnu_source_prefix + ''' 2078 #include <sys/types.h> 2079 #include <sys/mman.h> 2080 #include <stddef.h> 2081 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }''') 2082missing_madvise_proto = false 2083if has_madvise 2084 # Some platforms (illumos and Solaris before Solaris 11) provide madvise() 2085 # but forget to prototype it. In this case, has_madvise will be true (the 2086 # test program links despite a compile warning). To detect the 2087 # missing-prototype case, we try again with a definitely-bogus prototype. 2088 # This will only compile if the system headers don't provide the prototype; 2089 # otherwise the conflicting prototypes will cause a compiler error. 2090 missing_madvise_proto = cc.links(gnu_source_prefix + ''' 2091 #include <sys/types.h> 2092 #include <sys/mman.h> 2093 #include <stddef.h> 2094 extern int madvise(int); 2095 int main(void) { return madvise(0); }''') 2096endif 2097config_host_data.set('CONFIG_MADVISE', has_madvise) 2098config_host_data.set('HAVE_MADVISE_WITHOUT_PROTOTYPE', missing_madvise_proto) 2099 2100config_host_data.set('CONFIG_MEMFD', cc.links(gnu_source_prefix + ''' 2101 #include <sys/mman.h> 2102 int main(void) { return memfd_create("foo", MFD_ALLOW_SEALING); }''')) 2103config_host_data.set('CONFIG_OPEN_BY_HANDLE', cc.links(gnu_source_prefix + ''' 2104 #include <fcntl.h> 2105 #if !defined(AT_EMPTY_PATH) 2106 # error missing definition 2107 #else 2108 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); } 2109 #endif''')) 2110config_host_data.set('CONFIG_POSIX_MADVISE', cc.links(gnu_source_prefix + ''' 2111 #include <sys/mman.h> 2112 #include <stddef.h> 2113 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }''')) 2114 2115config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_W_TID', cc.links(gnu_source_prefix + ''' 2116 #include <pthread.h> 2117 2118 static void *f(void *p) { return NULL; } 2119 int main(void) 2120 { 2121 pthread_t thread; 2122 pthread_create(&thread, 0, f, 0); 2123 pthread_setname_np(thread, "QEMU"); 2124 return 0; 2125 }''', dependencies: threads)) 2126config_host_data.set('CONFIG_PTHREAD_SETNAME_NP_WO_TID', cc.links(gnu_source_prefix + ''' 2127 #include <pthread.h> 2128 2129 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; } 2130 int main(void) 2131 { 2132 pthread_t thread; 2133 pthread_create(&thread, 0, f, 0); 2134 return 0; 2135 }''', dependencies: threads)) 2136config_host_data.set('CONFIG_PTHREAD_CONDATTR_SETCLOCK', cc.links(gnu_source_prefix + ''' 2137 #include <pthread.h> 2138 #include <time.h> 2139 2140 int main(void) 2141 { 2142 pthread_condattr_t attr 2143 pthread_condattr_init(&attr); 2144 pthread_condattr_setclock(&attr, CLOCK_MONOTONIC); 2145 return 0; 2146 }''', dependencies: threads)) 2147config_host_data.set('CONFIG_PTHREAD_AFFINITY_NP', cc.links(gnu_source_prefix + ''' 2148 #include <pthread.h> 2149 2150 static void *f(void *p) { return NULL; } 2151 int main(void) 2152 { 2153 int setsize = CPU_ALLOC_SIZE(64); 2154 pthread_t thread; 2155 cpu_set_t *cpuset; 2156 pthread_create(&thread, 0, f, 0); 2157 cpuset = CPU_ALLOC(64); 2158 CPU_ZERO_S(setsize, cpuset); 2159 pthread_setaffinity_np(thread, setsize, cpuset); 2160 pthread_getaffinity_np(thread, setsize, cpuset); 2161 CPU_FREE(cpuset); 2162 return 0; 2163 }''', dependencies: threads)) 2164config_host_data.set('CONFIG_SIGNALFD', cc.links(gnu_source_prefix + ''' 2165 #include <sys/signalfd.h> 2166 #include <stddef.h> 2167 int main(void) { return signalfd(-1, NULL, SFD_CLOEXEC); }''')) 2168config_host_data.set('CONFIG_SPLICE', cc.links(gnu_source_prefix + ''' 2169 #include <unistd.h> 2170 #include <fcntl.h> 2171 #include <limits.h> 2172 2173 int main(void) 2174 { 2175 int len, fd = 0; 2176 len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK); 2177 splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE); 2178 return 0; 2179 }''')) 2180 2181config_host_data.set('HAVE_MLOCKALL', cc.links(gnu_source_prefix + ''' 2182 #include <sys/mman.h> 2183 int main(void) { 2184 return mlockall(MCL_FUTURE); 2185 }''')) 2186 2187have_l2tpv3 = false 2188if get_option('l2tpv3').allowed() and have_system 2189 have_l2tpv3 = cc.has_type('struct mmsghdr', 2190 prefix: gnu_source_prefix + ''' 2191 #include <sys/socket.h> 2192 #include <linux/ip.h>''') 2193endif 2194config_host_data.set('CONFIG_L2TPV3', have_l2tpv3) 2195 2196have_netmap = false 2197if get_option('netmap').allowed() and have_system 2198 have_netmap = cc.compiles(''' 2199 #include <inttypes.h> 2200 #include <net/if.h> 2201 #include <net/netmap.h> 2202 #include <net/netmap_user.h> 2203 #if (NETMAP_API < 11) || (NETMAP_API > 15) 2204 #error 2205 #endif 2206 int main(void) { return 0; }''') 2207 if not have_netmap and get_option('netmap').enabled() 2208 error('Netmap headers not available') 2209 endif 2210endif 2211config_host_data.set('CONFIG_NETMAP', have_netmap) 2212 2213# Work around a system header bug with some kernel/XFS header 2214# versions where they both try to define 'struct fsxattr': 2215# xfs headers will not try to redefine structs from linux headers 2216# if this macro is set. 2217config_host_data.set('HAVE_FSXATTR', cc.links(''' 2218 #include <linux/fs.h> 2219 struct fsxattr foo; 2220 int main(void) { 2221 return 0; 2222 }''')) 2223 2224# Some versions of Mac OS X incorrectly define SIZE_MAX 2225config_host_data.set('HAVE_BROKEN_SIZE_MAX', not cc.compiles(''' 2226 #include <stdint.h> 2227 #include <stdio.h> 2228 int main(void) { 2229 return printf("%zu", SIZE_MAX); 2230 }''', args: ['-Werror'])) 2231 2232atomic_test = ''' 2233 #include <stdint.h> 2234 int main(void) 2235 { 2236 @0@ x = 0, y = 0; 2237 y = __atomic_load_n(&x, __ATOMIC_RELAXED); 2238 __atomic_store_n(&x, y, __ATOMIC_RELAXED); 2239 __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED); 2240 __atomic_exchange_n(&x, y, __ATOMIC_RELAXED); 2241 __atomic_fetch_add(&x, y, __ATOMIC_RELAXED); 2242 return 0; 2243 }''' 2244 2245# See if 64-bit atomic operations are supported. 2246# Note that without __atomic builtins, we can only 2247# assume atomic loads/stores max at pointer size. 2248config_host_data.set('CONFIG_ATOMIC64', cc.links(atomic_test.format('uint64_t'))) 2249 2250has_int128 = cc.links(''' 2251 __int128_t a; 2252 __uint128_t b; 2253 int main (void) { 2254 a = a + b; 2255 b = a * b; 2256 a = a * a; 2257 return 0; 2258 }''') 2259 2260config_host_data.set('CONFIG_INT128', has_int128) 2261 2262if has_int128 2263 # "do we have 128-bit atomics which are handled inline and specifically not 2264 # via libatomic". The reason we can't use libatomic is documented in the 2265 # comment starting "GCC is a house divided" in include/qemu/atomic128.h. 2266 has_atomic128 = cc.links(atomic_test.format('unsigned __int128')) 2267 2268 config_host_data.set('CONFIG_ATOMIC128', has_atomic128) 2269 2270 if not has_atomic128 2271 has_cmpxchg128 = cc.links(''' 2272 int main(void) 2273 { 2274 unsigned __int128 x = 0, y = 0; 2275 __sync_val_compare_and_swap_16(&x, y, x); 2276 return 0; 2277 } 2278 ''') 2279 2280 config_host_data.set('CONFIG_CMPXCHG128', has_cmpxchg128) 2281 endif 2282endif 2283 2284config_host_data.set('CONFIG_GETAUXVAL', cc.links(gnu_source_prefix + ''' 2285 #include <sys/auxv.h> 2286 int main(void) { 2287 return getauxval(AT_HWCAP) == 0; 2288 }''')) 2289 2290config_host_data.set('CONFIG_USBFS', have_linux_user and cc.compiles(''' 2291 #include <linux/usbdevice_fs.h> 2292 2293 #ifndef USBDEVFS_GET_CAPABILITIES 2294 #error "USBDEVFS_GET_CAPABILITIES undefined" 2295 #endif 2296 2297 #ifndef USBDEVFS_DISCONNECT_CLAIM 2298 #error "USBDEVFS_DISCONNECT_CLAIM undefined" 2299 #endif 2300 2301 int main(void) { return 0; }''')) 2302 2303have_keyring = get_option('keyring') \ 2304 .require(targetos == 'linux', error_message: 'keyring is only available on Linux') \ 2305 .require(cc.compiles(''' 2306 #include <errno.h> 2307 #include <asm/unistd.h> 2308 #include <linux/keyctl.h> 2309 #include <sys/syscall.h> 2310 #include <unistd.h> 2311 int main(void) { 2312 return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0); 2313 }'''), error_message: 'keyctl syscall not available on this system').allowed() 2314config_host_data.set('CONFIG_SECRET_KEYRING', have_keyring) 2315 2316have_cpuid_h = cc.links(''' 2317 #include <cpuid.h> 2318 int main(void) { 2319 unsigned a, b, c, d; 2320 unsigned max = __get_cpuid_max(0, 0); 2321 2322 if (max >= 1) { 2323 __cpuid(1, a, b, c, d); 2324 } 2325 2326 if (max >= 7) { 2327 __cpuid_count(7, 0, a, b, c, d); 2328 } 2329 2330 return 0; 2331 }''') 2332config_host_data.set('CONFIG_CPUID_H', have_cpuid_h) 2333 2334config_host_data.set('CONFIG_AVX2_OPT', get_option('avx2') \ 2335 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX2') \ 2336 .require(cc.links(''' 2337 #include <cpuid.h> 2338 #include <immintrin.h> 2339 static int __attribute__((target("avx2"))) bar(void *a) { 2340 __m256i x = *(__m256i *)a; 2341 return _mm256_testz_si256(x, x); 2342 } 2343 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); } 2344 '''), error_message: 'AVX2 not available').allowed()) 2345 2346config_host_data.set('CONFIG_AVX512F_OPT', get_option('avx512f') \ 2347 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512F') \ 2348 .require(cc.links(''' 2349 #include <cpuid.h> 2350 #include <immintrin.h> 2351 static int __attribute__((target("avx512f"))) bar(void *a) { 2352 __m512i x = *(__m512i *)a; 2353 return _mm512_test_epi64_mask(x, x); 2354 } 2355 int main(int argc, char *argv[]) { return bar(argv[argc - 1]); } 2356 '''), error_message: 'AVX512F not available').allowed()) 2357 2358config_host_data.set('CONFIG_AVX512BW_OPT', get_option('avx512bw') \ 2359 .require(have_cpuid_h, error_message: 'cpuid.h not available, cannot enable AVX512BW') \ 2360 .require(cc.links(''' 2361 #pragma GCC push_options 2362 #pragma GCC target("avx512bw") 2363 #include <cpuid.h> 2364 #include <immintrin.h> 2365 static int bar(void *a) { 2366 2367 __m512i *x = a; 2368 __m512i res= _mm512_abs_epi8(*x); 2369 return res[1]; 2370 } 2371 int main(int argc, char *argv[]) { return bar(argv[0]); } 2372 '''), error_message: 'AVX512BW not available').allowed()) 2373 2374have_pvrdma = get_option('pvrdma') \ 2375 .require(rdma.found(), error_message: 'PVRDMA requires OpenFabrics libraries') \ 2376 .require(cc.compiles(gnu_source_prefix + ''' 2377 #include <sys/mman.h> 2378 int main(void) 2379 { 2380 char buf = 0; 2381 void *addr = &buf; 2382 addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED); 2383 2384 return 0; 2385 }'''), error_message: 'PVRDMA requires mremap').allowed() 2386 2387if have_pvrdma 2388 config_host_data.set('LEGACY_RDMA_REG_MR', not cc.links(''' 2389 #include <infiniband/verbs.h> 2390 int main(void) 2391 { 2392 struct ibv_mr *mr; 2393 struct ibv_pd *pd = NULL; 2394 size_t length = 10; 2395 uint64_t iova = 0; 2396 int access = 0; 2397 void *addr = NULL; 2398 2399 mr = ibv_reg_mr_iova(pd, addr, length, iova, access); 2400 ibv_dereg_mr(mr); 2401 return 0; 2402 }''')) 2403endif 2404 2405if get_option('membarrier').disabled() 2406 have_membarrier = false 2407elif targetos == 'windows' 2408 have_membarrier = true 2409elif targetos == 'linux' 2410 have_membarrier = cc.compiles(''' 2411 #include <linux/membarrier.h> 2412 #include <sys/syscall.h> 2413 #include <unistd.h> 2414 #include <stdlib.h> 2415 int main(void) { 2416 syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0); 2417 syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0); 2418 exit(0); 2419 }''') 2420endif 2421config_host_data.set('CONFIG_MEMBARRIER', get_option('membarrier') \ 2422 .require(have_membarrier, error_message: 'membarrier system call not available') \ 2423 .allowed()) 2424 2425have_afalg = get_option('crypto_afalg') \ 2426 .require(cc.compiles(gnu_source_prefix + ''' 2427 #include <errno.h> 2428 #include <sys/types.h> 2429 #include <sys/socket.h> 2430 #include <linux/if_alg.h> 2431 int main(void) { 2432 int sock; 2433 sock = socket(AF_ALG, SOCK_SEQPACKET, 0); 2434 return sock; 2435 } 2436 '''), error_message: 'AF_ALG requested but could not be detected').allowed() 2437config_host_data.set('CONFIG_AF_ALG', have_afalg) 2438 2439config_host_data.set('CONFIG_AF_VSOCK', cc.has_header_symbol( 2440 'linux/vm_sockets.h', 'AF_VSOCK', 2441 prefix: '#include <sys/socket.h>', 2442)) 2443 2444have_vss = false 2445have_vss_sdk = false # old xp/2003 SDK 2446if targetos == 'windows' and link_language == 'cpp' 2447 have_vss = cxx.compiles(''' 2448 #define __MIDL_user_allocate_free_DEFINED__ 2449 #include <vss.h> 2450 int main(void) { return VSS_CTX_BACKUP; }''') 2451 have_vss_sdk = cxx.has_header('vscoordint.h') 2452endif 2453config_host_data.set('HAVE_VSS_SDK', have_vss_sdk) 2454 2455foreach k, v: config_host 2456 if k.startswith('CONFIG_') 2457 config_host_data.set(k, v == 'y' ? 1 : v) 2458 endif 2459endforeach 2460 2461# Older versions of MinGW do not import _lock_file and _unlock_file properly. 2462# This was fixed for v6.0.0 with commit b48e3ac8969d. 2463if targetos == 'windows' 2464 config_host_data.set('HAVE__LOCK_FILE', cc.links(''' 2465 #include <stdio.h> 2466 int main(void) { 2467 _lock_file(NULL); 2468 _unlock_file(NULL); 2469 return 0; 2470 }''', name: '_lock_file and _unlock_file')) 2471endif 2472 2473######################## 2474# Target configuration # 2475######################## 2476 2477minikconf = find_program('scripts/minikconf.py') 2478config_all = {} 2479config_all_devices = {} 2480config_all_disas = {} 2481config_devices_mak_list = [] 2482config_devices_h = {} 2483config_target_h = {} 2484config_target_mak = {} 2485 2486disassemblers = { 2487 'alpha' : ['CONFIG_ALPHA_DIS'], 2488 'avr' : ['CONFIG_AVR_DIS'], 2489 'cris' : ['CONFIG_CRIS_DIS'], 2490 'hexagon' : ['CONFIG_HEXAGON_DIS'], 2491 'hppa' : ['CONFIG_HPPA_DIS'], 2492 'i386' : ['CONFIG_I386_DIS'], 2493 'x86_64' : ['CONFIG_I386_DIS'], 2494 'm68k' : ['CONFIG_M68K_DIS'], 2495 'microblaze' : ['CONFIG_MICROBLAZE_DIS'], 2496 'mips' : ['CONFIG_MIPS_DIS'], 2497 'nios2' : ['CONFIG_NIOS2_DIS'], 2498 'or1k' : ['CONFIG_OPENRISC_DIS'], 2499 'ppc' : ['CONFIG_PPC_DIS'], 2500 'riscv' : ['CONFIG_RISCV_DIS'], 2501 'rx' : ['CONFIG_RX_DIS'], 2502 's390' : ['CONFIG_S390_DIS'], 2503 'sh4' : ['CONFIG_SH4_DIS'], 2504 'sparc' : ['CONFIG_SPARC_DIS'], 2505 'xtensa' : ['CONFIG_XTENSA_DIS'], 2506 'loongarch' : ['CONFIG_LOONGARCH_DIS'], 2507} 2508 2509have_ivshmem = config_host_data.get('CONFIG_EVENTFD') 2510host_kconfig = \ 2511 (get_option('fuzzing') ? ['CONFIG_FUZZ=y'] : []) + \ 2512 (have_tpm ? ['CONFIG_TPM=y'] : []) + \ 2513 (spice.found() ? ['CONFIG_SPICE=y'] : []) + \ 2514 (have_ivshmem ? ['CONFIG_IVSHMEM=y'] : []) + \ 2515 (opengl.found() ? ['CONFIG_OPENGL=y'] : []) + \ 2516 (x11.found() ? ['CONFIG_X11=y'] : []) + \ 2517 (have_vhost_user ? ['CONFIG_VHOST_USER=y'] : []) + \ 2518 (have_vhost_vdpa ? ['CONFIG_VHOST_VDPA=y'] : []) + \ 2519 (have_vhost_kernel ? ['CONFIG_VHOST_KERNEL=y'] : []) + \ 2520 (have_virtfs ? ['CONFIG_VIRTFS=y'] : []) + \ 2521 ('CONFIG_LINUX' in config_host ? ['CONFIG_LINUX=y'] : []) + \ 2522 (have_pvrdma ? ['CONFIG_PVRDMA=y'] : []) + \ 2523 (multiprocess_allowed ? ['CONFIG_MULTIPROCESS_ALLOWED=y'] : []) + \ 2524 (vfio_user_server_allowed ? ['CONFIG_VFIO_USER_SERVER_ALLOWED=y'] : []) 2525 2526ignored = [ 'TARGET_XML_FILES', 'TARGET_ABI_DIR', 'TARGET_ARCH' ] 2527 2528default_targets = 'CONFIG_DEFAULT_TARGETS' in config_host 2529actual_target_dirs = [] 2530fdt_required = [] 2531foreach target : target_dirs 2532 config_target = { 'TARGET_NAME': target.split('-')[0] } 2533 if target.endswith('linux-user') 2534 if targetos != 'linux' 2535 if default_targets 2536 continue 2537 endif 2538 error('Target @0@ is only available on a Linux host'.format(target)) 2539 endif 2540 config_target += { 'CONFIG_LINUX_USER': 'y' } 2541 elif target.endswith('bsd-user') 2542 if 'CONFIG_BSD' not in config_host 2543 if default_targets 2544 continue 2545 endif 2546 error('Target @0@ is only available on a BSD host'.format(target)) 2547 endif 2548 config_target += { 'CONFIG_BSD_USER': 'y' } 2549 elif target.endswith('softmmu') 2550 config_target += { 'CONFIG_SOFTMMU': 'y' } 2551 endif 2552 if target.endswith('-user') 2553 config_target += { 2554 'CONFIG_USER_ONLY': 'y', 2555 'CONFIG_QEMU_INTERP_PREFIX': 2556 get_option('interp_prefix').replace('%M', config_target['TARGET_NAME']) 2557 } 2558 endif 2559 2560 accel_kconfig = [] 2561 foreach sym: accelerators 2562 if sym == 'CONFIG_TCG' or target in accelerator_targets.get(sym, []) 2563 config_target += { sym: 'y' } 2564 config_all += { sym: 'y' } 2565 if target in modular_tcg 2566 config_target += { 'CONFIG_TCG_MODULAR': 'y' } 2567 else 2568 config_target += { 'CONFIG_TCG_BUILTIN': 'y' } 2569 endif 2570 accel_kconfig += [ sym + '=y' ] 2571 endif 2572 endforeach 2573 if accel_kconfig.length() == 0 2574 if default_targets 2575 continue 2576 endif 2577 error('No accelerator available for target @0@'.format(target)) 2578 endif 2579 2580 actual_target_dirs += target 2581 config_target += keyval.load('configs/targets' / target + '.mak') 2582 config_target += { 'TARGET_' + config_target['TARGET_ARCH'].to_upper(): 'y' } 2583 2584 if 'TARGET_NEED_FDT' in config_target 2585 fdt_required += target 2586 endif 2587 2588 # Add default keys 2589 if 'TARGET_BASE_ARCH' not in config_target 2590 config_target += {'TARGET_BASE_ARCH': config_target['TARGET_ARCH']} 2591 endif 2592 if 'TARGET_ABI_DIR' not in config_target 2593 config_target += {'TARGET_ABI_DIR': config_target['TARGET_ARCH']} 2594 endif 2595 if 'TARGET_BIG_ENDIAN' not in config_target 2596 config_target += {'TARGET_BIG_ENDIAN': 'n'} 2597 endif 2598 2599 foreach k, v: disassemblers 2600 if host_arch.startswith(k) or config_target['TARGET_BASE_ARCH'].startswith(k) 2601 foreach sym: v 2602 config_target += { sym: 'y' } 2603 config_all_disas += { sym: 'y' } 2604 endforeach 2605 endif 2606 endforeach 2607 2608 config_target_data = configuration_data() 2609 foreach k, v: config_target 2610 if not k.startswith('TARGET_') and not k.startswith('CONFIG_') 2611 # do nothing 2612 elif ignored.contains(k) 2613 # do nothing 2614 elif k == 'TARGET_BASE_ARCH' 2615 # Note that TARGET_BASE_ARCH ends up in config-target.h but it is 2616 # not used to select files from sourcesets. 2617 config_target_data.set('TARGET_' + v.to_upper(), 1) 2618 elif k == 'TARGET_NAME' or k == 'CONFIG_QEMU_INTERP_PREFIX' 2619 config_target_data.set_quoted(k, v) 2620 elif v == 'y' 2621 config_target_data.set(k, 1) 2622 elif v == 'n' 2623 config_target_data.set(k, 0) 2624 else 2625 config_target_data.set(k, v) 2626 endif 2627 endforeach 2628 config_target_data.set('QEMU_ARCH', 2629 'QEMU_ARCH_' + config_target['TARGET_BASE_ARCH'].to_upper()) 2630 config_target_h += {target: configure_file(output: target + '-config-target.h', 2631 configuration: config_target_data)} 2632 2633 if target.endswith('-softmmu') 2634 config_input = meson.get_external_property(target, 'default') 2635 config_devices_mak = target + '-config-devices.mak' 2636 config_devices_mak = configure_file( 2637 input: ['configs/devices' / target / config_input + '.mak', 'Kconfig'], 2638 output: config_devices_mak, 2639 depfile: config_devices_mak + '.d', 2640 capture: true, 2641 command: [minikconf, 2642 get_option('default_devices') ? '--defconfig' : '--allnoconfig', 2643 config_devices_mak, '@DEPFILE@', '@INPUT@', 2644 host_kconfig, accel_kconfig, 2645 'CONFIG_' + config_target['TARGET_ARCH'].to_upper() + '=y']) 2646 2647 config_devices_data = configuration_data() 2648 config_devices = keyval.load(config_devices_mak) 2649 foreach k, v: config_devices 2650 config_devices_data.set(k, 1) 2651 endforeach 2652 config_devices_mak_list += config_devices_mak 2653 config_devices_h += {target: configure_file(output: target + '-config-devices.h', 2654 configuration: config_devices_data)} 2655 config_target += config_devices 2656 config_all_devices += config_devices 2657 endif 2658 config_target_mak += {target: config_target} 2659endforeach 2660target_dirs = actual_target_dirs 2661 2662# This configuration is used to build files that are shared by 2663# multiple binaries, and then extracted out of the "common" 2664# static_library target. 2665# 2666# We do not use all_sources()/all_dependencies(), because it would 2667# build literally all source files, including devices only used by 2668# targets that are not built for this compilation. The CONFIG_ALL 2669# pseudo symbol replaces it. 2670 2671config_all += config_all_devices 2672config_all += config_host 2673config_all += config_all_disas 2674config_all += { 2675 'CONFIG_XEN': xen.found(), 2676 'CONFIG_SOFTMMU': have_system, 2677 'CONFIG_USER_ONLY': have_user, 2678 'CONFIG_ALL': true, 2679} 2680 2681target_configs_h = [] 2682foreach target: target_dirs 2683 target_configs_h += config_target_h[target] 2684 target_configs_h += config_devices_h.get(target, []) 2685endforeach 2686genh += custom_target('config-poison.h', 2687 input: [target_configs_h], 2688 output: 'config-poison.h', 2689 capture: true, 2690 command: [find_program('scripts/make-config-poison.sh'), 2691 target_configs_h]) 2692 2693############## 2694# Submodules # 2695############## 2696 2697capstone = not_found 2698if not get_option('capstone').auto() or have_system or have_user 2699 capstone = dependency('capstone', version: '>=3.0.5', 2700 kwargs: static_kwargs, method: 'pkg-config', 2701 required: get_option('capstone')) 2702 2703 # Some versions of capstone have broken pkg-config file 2704 # that reports a wrong -I path, causing the #include to 2705 # fail later. If the system has such a broken version 2706 # do not use it. 2707 if capstone.found() and not cc.compiles('#include <capstone.h>', 2708 dependencies: [capstone]) 2709 capstone = not_found 2710 if get_option('capstone').enabled() 2711 error('capstone requested, but it does not appear to work') 2712 endif 2713 endif 2714endif 2715 2716libvfio_user_dep = not_found 2717if have_system and vfio_user_server_allowed 2718 have_internal = fs.exists(meson.current_source_dir() / 'subprojects/libvfio-user/meson.build') 2719 2720 if not have_internal 2721 error('libvfio-user source not found - please pull git submodule') 2722 endif 2723 2724 libvfio_user_proj = subproject('libvfio-user') 2725 2726 libvfio_user_lib = libvfio_user_proj.get_variable('libvfio_user_dep') 2727 2728 libvfio_user_dep = declare_dependency(dependencies: [libvfio_user_lib]) 2729endif 2730 2731fdt = not_found 2732if have_system 2733 fdt_opt = get_option('fdt') 2734 if fdt_opt in ['enabled', 'auto', 'system'] 2735 have_internal = fs.exists(meson.current_source_dir() / 'dtc/libfdt/Makefile.libfdt') 2736 fdt = cc.find_library('fdt', kwargs: static_kwargs, 2737 required: fdt_opt == 'system' or 2738 fdt_opt == 'enabled' and not have_internal) 2739 if fdt.found() and cc.links(''' 2740 #include <libfdt.h> 2741 #include <libfdt_env.h> 2742 int main(void) { fdt_find_max_phandle(NULL, NULL); return 0; }''', 2743 dependencies: fdt) 2744 fdt_opt = 'system' 2745 elif fdt_opt == 'system' 2746 error('system libfdt requested, but it is too old (1.5.1 or newer required)') 2747 elif have_internal 2748 fdt_opt = 'internal' 2749 else 2750 fdt_opt = 'disabled' 2751 fdt = not_found 2752 endif 2753 endif 2754 if fdt_opt == 'internal' 2755 fdt_files = files( 2756 'dtc/libfdt/fdt.c', 2757 'dtc/libfdt/fdt_ro.c', 2758 'dtc/libfdt/fdt_wip.c', 2759 'dtc/libfdt/fdt_sw.c', 2760 'dtc/libfdt/fdt_rw.c', 2761 'dtc/libfdt/fdt_strerror.c', 2762 'dtc/libfdt/fdt_empty_tree.c', 2763 'dtc/libfdt/fdt_addresses.c', 2764 'dtc/libfdt/fdt_overlay.c', 2765 'dtc/libfdt/fdt_check.c', 2766 ) 2767 2768 fdt_inc = include_directories('dtc/libfdt') 2769 libfdt = static_library('fdt', 2770 build_by_default: false, 2771 sources: fdt_files, 2772 include_directories: fdt_inc) 2773 fdt = declare_dependency(link_with: libfdt, 2774 include_directories: fdt_inc) 2775 endif 2776else 2777 fdt_opt = 'disabled' 2778endif 2779if not fdt.found() and fdt_required.length() > 0 2780 error('fdt not available but required by targets ' + ', '.join(fdt_required)) 2781endif 2782 2783config_host_data.set('CONFIG_CAPSTONE', capstone.found()) 2784config_host_data.set('CONFIG_FDT', fdt.found()) 2785config_host_data.set('CONFIG_SLIRP', slirp.found()) 2786 2787##################### 2788# Generated sources # 2789##################### 2790 2791genh += configure_file(output: 'config-host.h', configuration: config_host_data) 2792 2793hxtool = find_program('scripts/hxtool') 2794shaderinclude = find_program('scripts/shaderinclude.py') 2795qapi_gen = find_program('scripts/qapi-gen.py') 2796qapi_gen_depends = [ meson.current_source_dir() / 'scripts/qapi/__init__.py', 2797 meson.current_source_dir() / 'scripts/qapi/commands.py', 2798 meson.current_source_dir() / 'scripts/qapi/common.py', 2799 meson.current_source_dir() / 'scripts/qapi/error.py', 2800 meson.current_source_dir() / 'scripts/qapi/events.py', 2801 meson.current_source_dir() / 'scripts/qapi/expr.py', 2802 meson.current_source_dir() / 'scripts/qapi/gen.py', 2803 meson.current_source_dir() / 'scripts/qapi/introspect.py', 2804 meson.current_source_dir() / 'scripts/qapi/parser.py', 2805 meson.current_source_dir() / 'scripts/qapi/schema.py', 2806 meson.current_source_dir() / 'scripts/qapi/source.py', 2807 meson.current_source_dir() / 'scripts/qapi/types.py', 2808 meson.current_source_dir() / 'scripts/qapi/visit.py', 2809 meson.current_source_dir() / 'scripts/qapi/common.py', 2810 meson.current_source_dir() / 'scripts/qapi-gen.py' 2811] 2812 2813tracetool = [ 2814 python, files('scripts/tracetool.py'), 2815 '--backend=' + ','.join(get_option('trace_backends')) 2816] 2817tracetool_depends = files( 2818 'scripts/tracetool/backend/log.py', 2819 'scripts/tracetool/backend/__init__.py', 2820 'scripts/tracetool/backend/dtrace.py', 2821 'scripts/tracetool/backend/ftrace.py', 2822 'scripts/tracetool/backend/simple.py', 2823 'scripts/tracetool/backend/syslog.py', 2824 'scripts/tracetool/backend/ust.py', 2825 'scripts/tracetool/format/ust_events_c.py', 2826 'scripts/tracetool/format/ust_events_h.py', 2827 'scripts/tracetool/format/__init__.py', 2828 'scripts/tracetool/format/d.py', 2829 'scripts/tracetool/format/simpletrace_stap.py', 2830 'scripts/tracetool/format/c.py', 2831 'scripts/tracetool/format/h.py', 2832 'scripts/tracetool/format/log_stap.py', 2833 'scripts/tracetool/format/stap.py', 2834 'scripts/tracetool/__init__.py', 2835 'scripts/tracetool/transform.py', 2836 'scripts/tracetool/vcpu.py' 2837) 2838 2839qemu_version_cmd = [find_program('scripts/qemu-version.sh'), 2840 meson.current_source_dir(), 2841 get_option('pkgversion'), meson.project_version()] 2842qemu_version = custom_target('qemu-version.h', 2843 output: 'qemu-version.h', 2844 command: qemu_version_cmd, 2845 capture: true, 2846 build_by_default: true, 2847 build_always_stale: true) 2848genh += qemu_version 2849 2850hxdep = [] 2851hx_headers = [ 2852 ['qemu-options.hx', 'qemu-options.def'], 2853 ['qemu-img-cmds.hx', 'qemu-img-cmds.h'], 2854] 2855if have_system 2856 hx_headers += [ 2857 ['hmp-commands.hx', 'hmp-commands.h'], 2858 ['hmp-commands-info.hx', 'hmp-commands-info.h'], 2859 ] 2860endif 2861foreach d : hx_headers 2862 hxdep += custom_target(d[1], 2863 input: files(d[0]), 2864 output: d[1], 2865 capture: true, 2866 build_by_default: true, # to be removed when added to a target 2867 command: [hxtool, '-h', '@INPUT0@']) 2868endforeach 2869genh += hxdep 2870 2871################### 2872# Collect sources # 2873################### 2874 2875authz_ss = ss.source_set() 2876blockdev_ss = ss.source_set() 2877block_ss = ss.source_set() 2878chardev_ss = ss.source_set() 2879common_ss = ss.source_set() 2880crypto_ss = ss.source_set() 2881hwcore_ss = ss.source_set() 2882io_ss = ss.source_set() 2883qmp_ss = ss.source_set() 2884qom_ss = ss.source_set() 2885softmmu_ss = ss.source_set() 2886specific_fuzz_ss = ss.source_set() 2887specific_ss = ss.source_set() 2888stub_ss = ss.source_set() 2889trace_ss = ss.source_set() 2890user_ss = ss.source_set() 2891util_ss = ss.source_set() 2892 2893# accel modules 2894qtest_module_ss = ss.source_set() 2895tcg_module_ss = ss.source_set() 2896 2897modules = {} 2898target_modules = {} 2899hw_arch = {} 2900target_arch = {} 2901target_softmmu_arch = {} 2902target_user_arch = {} 2903 2904############### 2905# Trace files # 2906############### 2907 2908# TODO: add each directory to the subdirs from its own meson.build, once 2909# we have those 2910trace_events_subdirs = [ 2911 'crypto', 2912 'qapi', 2913 'qom', 2914 'monitor', 2915 'util', 2916 'gdbstub', 2917] 2918if have_linux_user 2919 trace_events_subdirs += [ 'linux-user' ] 2920endif 2921if have_bsd_user 2922 trace_events_subdirs += [ 'bsd-user' ] 2923endif 2924if have_block 2925 trace_events_subdirs += [ 2926 'authz', 2927 'block', 2928 'io', 2929 'nbd', 2930 'scsi', 2931 ] 2932endif 2933if have_system 2934 trace_events_subdirs += [ 2935 'accel/kvm', 2936 'audio', 2937 'backends', 2938 'backends/tpm', 2939 'chardev', 2940 'ebpf', 2941 'hw/9pfs', 2942 'hw/acpi', 2943 'hw/adc', 2944 'hw/alpha', 2945 'hw/arm', 2946 'hw/audio', 2947 'hw/block', 2948 'hw/block/dataplane', 2949 'hw/char', 2950 'hw/display', 2951 'hw/dma', 2952 'hw/hyperv', 2953 'hw/i2c', 2954 'hw/i386', 2955 'hw/i386/xen', 2956 'hw/ide', 2957 'hw/input', 2958 'hw/intc', 2959 'hw/isa', 2960 'hw/mem', 2961 'hw/mips', 2962 'hw/misc', 2963 'hw/misc/macio', 2964 'hw/net', 2965 'hw/net/can', 2966 'hw/nubus', 2967 'hw/nvme', 2968 'hw/nvram', 2969 'hw/pci', 2970 'hw/pci-host', 2971 'hw/ppc', 2972 'hw/rdma', 2973 'hw/rdma/vmw', 2974 'hw/rtc', 2975 'hw/s390x', 2976 'hw/scsi', 2977 'hw/sd', 2978 'hw/sh4', 2979 'hw/sparc', 2980 'hw/sparc64', 2981 'hw/ssi', 2982 'hw/timer', 2983 'hw/tpm', 2984 'hw/usb', 2985 'hw/vfio', 2986 'hw/virtio', 2987 'hw/watchdog', 2988 'hw/xen', 2989 'hw/gpio', 2990 'migration', 2991 'net', 2992 'softmmu', 2993 'ui', 2994 'hw/remote', 2995 ] 2996endif 2997if have_system or have_user 2998 trace_events_subdirs += [ 2999 'accel/tcg', 3000 'hw/core', 3001 'target/arm', 3002 'target/arm/hvf', 3003 'target/hppa', 3004 'target/i386', 3005 'target/i386/kvm', 3006 'target/mips/tcg', 3007 'target/nios2', 3008 'target/ppc', 3009 'target/riscv', 3010 'target/s390x', 3011 'target/s390x/kvm', 3012 'target/sparc', 3013 ] 3014endif 3015 3016vhost_user = not_found 3017if targetos == 'linux' and have_vhost_user 3018 libvhost_user = subproject('libvhost-user') 3019 vhost_user = libvhost_user.get_variable('vhost_user_dep') 3020endif 3021 3022libvduse = not_found 3023if have_libvduse 3024 libvduse_proj = subproject('libvduse') 3025 libvduse = libvduse_proj.get_variable('libvduse_dep') 3026endif 3027 3028# NOTE: the trace/ subdirectory needs the qapi_trace_events variable 3029# that is filled in by qapi/. 3030subdir('qapi') 3031subdir('qobject') 3032subdir('stubs') 3033subdir('trace') 3034subdir('util') 3035subdir('qom') 3036subdir('authz') 3037subdir('crypto') 3038subdir('ui') 3039subdir('hw') 3040subdir('gdbstub') 3041 3042 3043if enable_modules 3044 libmodulecommon = static_library('module-common', files('module-common.c') + genh, pic: true, c_args: '-DBUILD_DSO') 3045 modulecommon = declare_dependency(link_whole: libmodulecommon, compile_args: '-DBUILD_DSO') 3046endif 3047 3048qom_ss = qom_ss.apply(config_host, strict: false) 3049libqom = static_library('qom', qom_ss.sources() + genh, 3050 dependencies: [qom_ss.dependencies()], 3051 name_suffix: 'fa') 3052qom = declare_dependency(link_whole: libqom) 3053 3054event_loop_base = files('event-loop-base.c') 3055event_loop_base = static_library('event-loop-base', sources: event_loop_base + genh, 3056 build_by_default: true) 3057event_loop_base = declare_dependency(link_whole: event_loop_base, 3058 dependencies: [qom]) 3059 3060stub_ss = stub_ss.apply(config_all, strict: false) 3061 3062util_ss.add_all(trace_ss) 3063util_ss = util_ss.apply(config_all, strict: false) 3064libqemuutil = static_library('qemuutil', 3065 sources: util_ss.sources() + stub_ss.sources() + genh, 3066 dependencies: [util_ss.dependencies(), libm, threads, glib, socket, malloc, pixman]) 3067qemuutil = declare_dependency(link_with: libqemuutil, 3068 sources: genh + version_res, 3069 dependencies: [event_loop_base]) 3070 3071if have_system or have_user 3072 decodetree = generator(find_program('scripts/decodetree.py'), 3073 output: 'decode-@BASENAME@.c.inc', 3074 arguments: ['@INPUT@', '@EXTRA_ARGS@', '-o', '@OUTPUT@']) 3075 subdir('libdecnumber') 3076 subdir('target') 3077endif 3078 3079subdir('audio') 3080subdir('io') 3081subdir('chardev') 3082subdir('fsdev') 3083subdir('dump') 3084 3085if have_block 3086 block_ss.add(files( 3087 'block.c', 3088 'blockjob.c', 3089 'job.c', 3090 'qemu-io-cmds.c', 3091 )) 3092 if config_host_data.get('CONFIG_REPLICATION') 3093 block_ss.add(files('replication.c')) 3094 endif 3095 3096 subdir('nbd') 3097 subdir('scsi') 3098 subdir('block') 3099 3100 blockdev_ss.add(files( 3101 'blockdev.c', 3102 'blockdev-nbd.c', 3103 'iothread.c', 3104 'job-qmp.c', 3105 ), gnutls) 3106 3107 # os-posix.c contains POSIX-specific functions used by qemu-storage-daemon, 3108 # os-win32.c does not 3109 blockdev_ss.add(when: 'CONFIG_POSIX', if_true: files('os-posix.c')) 3110 softmmu_ss.add(when: 'CONFIG_WIN32', if_true: [files('os-win32.c')]) 3111endif 3112 3113common_ss.add(files('cpus-common.c')) 3114 3115subdir('softmmu') 3116 3117common_ss.add(capstone) 3118specific_ss.add(files('cpu.c', 'disas.c'), capstone) 3119 3120# Work around a gcc bug/misfeature wherein constant propagation looks 3121# through an alias: 3122# https://gcc.gnu.org/bugzilla/show_bug.cgi?id=99696 3123# to guess that a const variable is always zero. Without lto, this is 3124# impossible, as the alias is restricted to page-vary-common.c. Indeed, 3125# without lto, not even the alias is required -- we simply use different 3126# declarations in different compilation units. 3127pagevary = files('page-vary-common.c') 3128if get_option('b_lto') 3129 pagevary_flags = ['-fno-lto'] 3130 if get_option('cfi') 3131 pagevary_flags += '-fno-sanitize=cfi-icall' 3132 endif 3133 pagevary = static_library('page-vary-common', sources: pagevary + genh, 3134 c_args: pagevary_flags) 3135 pagevary = declare_dependency(link_with: pagevary) 3136endif 3137common_ss.add(pagevary) 3138specific_ss.add(files('page-vary.c')) 3139 3140subdir('backends') 3141subdir('disas') 3142subdir('migration') 3143subdir('monitor') 3144subdir('net') 3145subdir('replay') 3146subdir('semihosting') 3147subdir('stats') 3148subdir('tcg') 3149subdir('fpu') 3150subdir('accel') 3151subdir('plugins') 3152subdir('ebpf') 3153 3154common_user_inc = [] 3155 3156subdir('common-user') 3157subdir('bsd-user') 3158subdir('linux-user') 3159 3160# needed for fuzzing binaries 3161subdir('tests/qtest/libqos') 3162subdir('tests/qtest/fuzz') 3163 3164# accel modules 3165tcg_real_module_ss = ss.source_set() 3166tcg_real_module_ss.add_all(when: 'CONFIG_TCG_MODULAR', if_true: tcg_module_ss) 3167specific_ss.add_all(when: 'CONFIG_TCG_BUILTIN', if_true: tcg_module_ss) 3168target_modules += { 'accel' : { 'qtest': qtest_module_ss, 3169 'tcg': tcg_real_module_ss }} 3170 3171######################## 3172# Library dependencies # 3173######################## 3174 3175modinfo_collect = find_program('scripts/modinfo-collect.py') 3176modinfo_generate = find_program('scripts/modinfo-generate.py') 3177modinfo_files = [] 3178 3179block_mods = [] 3180softmmu_mods = [] 3181foreach d, list : modules 3182 foreach m, module_ss : list 3183 if enable_modules and targetos != 'windows' 3184 module_ss = module_ss.apply(config_all, strict: false) 3185 sl = static_library(d + '-' + m, [genh, module_ss.sources()], 3186 dependencies: [modulecommon, module_ss.dependencies()], pic: true) 3187 if d == 'block' 3188 block_mods += sl 3189 else 3190 softmmu_mods += sl 3191 endif 3192 if module_ss.sources() != [] 3193 # FIXME: Should use sl.extract_all_objects(recursive: true) as 3194 # input. Sources can be used multiple times but objects are 3195 # unique when it comes to lookup in compile_commands.json. 3196 # Depnds on a mesion version with 3197 # https://github.com/mesonbuild/meson/pull/8900 3198 modinfo_files += custom_target(d + '-' + m + '.modinfo', 3199 output: d + '-' + m + '.modinfo', 3200 input: module_ss.sources() + genh, 3201 capture: true, 3202 command: [modinfo_collect, module_ss.sources()]) 3203 endif 3204 else 3205 if d == 'block' 3206 block_ss.add_all(module_ss) 3207 else 3208 softmmu_ss.add_all(module_ss) 3209 endif 3210 endif 3211 endforeach 3212endforeach 3213 3214foreach d, list : target_modules 3215 foreach m, module_ss : list 3216 if enable_modules and targetos != 'windows' 3217 foreach target : target_dirs 3218 if target.endswith('-softmmu') 3219 config_target = config_target_mak[target] 3220 config_target += config_host 3221 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])] 3222 c_args = ['-DNEED_CPU_H', 3223 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target), 3224 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)] 3225 target_module_ss = module_ss.apply(config_target, strict: false) 3226 if target_module_ss.sources() != [] 3227 module_name = d + '-' + m + '-' + config_target['TARGET_NAME'] 3228 sl = static_library(module_name, 3229 [genh, target_module_ss.sources()], 3230 dependencies: [modulecommon, target_module_ss.dependencies()], 3231 include_directories: target_inc, 3232 c_args: c_args, 3233 pic: true) 3234 softmmu_mods += sl 3235 # FIXME: Should use sl.extract_all_objects(recursive: true) too. 3236 modinfo_files += custom_target(module_name + '.modinfo', 3237 output: module_name + '.modinfo', 3238 input: target_module_ss.sources() + genh, 3239 capture: true, 3240 command: [modinfo_collect, '--target', target, target_module_ss.sources()]) 3241 endif 3242 endif 3243 endforeach 3244 else 3245 specific_ss.add_all(module_ss) 3246 endif 3247 endforeach 3248endforeach 3249 3250if enable_modules 3251 foreach target : target_dirs 3252 if target.endswith('-softmmu') 3253 config_target = config_target_mak[target] 3254 config_devices_mak = target + '-config-devices.mak' 3255 modinfo_src = custom_target('modinfo-' + target + '.c', 3256 output: 'modinfo-' + target + '.c', 3257 input: modinfo_files, 3258 command: [modinfo_generate, '--devices', config_devices_mak, '@INPUT@'], 3259 capture: true) 3260 3261 modinfo_lib = static_library('modinfo-' + target + '.c', modinfo_src) 3262 modinfo_dep = declare_dependency(link_with: modinfo_lib) 3263 3264 arch = config_target['TARGET_NAME'] == 'sparc64' ? 'sparc64' : config_target['TARGET_BASE_ARCH'] 3265 hw_arch[arch].add(modinfo_dep) 3266 endif 3267 endforeach 3268endif 3269 3270nm = find_program('nm') 3271undefsym = find_program('scripts/undefsym.py') 3272block_syms = custom_target('block.syms', output: 'block.syms', 3273 input: [libqemuutil, block_mods], 3274 capture: true, 3275 command: [undefsym, nm, '@INPUT@']) 3276qemu_syms = custom_target('qemu.syms', output: 'qemu.syms', 3277 input: [libqemuutil, softmmu_mods], 3278 capture: true, 3279 command: [undefsym, nm, '@INPUT@']) 3280 3281authz_ss = authz_ss.apply(config_host, strict: false) 3282libauthz = static_library('authz', authz_ss.sources() + genh, 3283 dependencies: [authz_ss.dependencies()], 3284 name_suffix: 'fa', 3285 build_by_default: false) 3286 3287authz = declare_dependency(link_whole: libauthz, 3288 dependencies: qom) 3289 3290crypto_ss = crypto_ss.apply(config_host, strict: false) 3291libcrypto = static_library('crypto', crypto_ss.sources() + genh, 3292 dependencies: [crypto_ss.dependencies()], 3293 name_suffix: 'fa', 3294 build_by_default: false) 3295 3296crypto = declare_dependency(link_whole: libcrypto, 3297 dependencies: [authz, qom]) 3298 3299io_ss = io_ss.apply(config_host, strict: false) 3300libio = static_library('io', io_ss.sources() + genh, 3301 dependencies: [io_ss.dependencies()], 3302 link_with: libqemuutil, 3303 name_suffix: 'fa', 3304 build_by_default: false) 3305 3306io = declare_dependency(link_whole: libio, dependencies: [crypto, qom]) 3307 3308libmigration = static_library('migration', sources: migration_files + genh, 3309 name_suffix: 'fa', 3310 build_by_default: false) 3311migration = declare_dependency(link_with: libmigration, 3312 dependencies: [zlib, qom, io]) 3313softmmu_ss.add(migration) 3314 3315block_ss = block_ss.apply(config_host, strict: false) 3316libblock = static_library('block', block_ss.sources() + genh, 3317 dependencies: block_ss.dependencies(), 3318 link_depends: block_syms, 3319 name_suffix: 'fa', 3320 build_by_default: false) 3321 3322block = declare_dependency(link_whole: [libblock], 3323 link_args: '@block.syms', 3324 dependencies: [crypto, io]) 3325 3326blockdev_ss = blockdev_ss.apply(config_host, strict: false) 3327libblockdev = static_library('blockdev', blockdev_ss.sources() + genh, 3328 dependencies: blockdev_ss.dependencies(), 3329 name_suffix: 'fa', 3330 build_by_default: false) 3331 3332blockdev = declare_dependency(link_whole: [libblockdev], 3333 dependencies: [block, event_loop_base]) 3334 3335qmp_ss = qmp_ss.apply(config_host, strict: false) 3336libqmp = static_library('qmp', qmp_ss.sources() + genh, 3337 dependencies: qmp_ss.dependencies(), 3338 name_suffix: 'fa', 3339 build_by_default: false) 3340 3341qmp = declare_dependency(link_whole: [libqmp]) 3342 3343libchardev = static_library('chardev', chardev_ss.sources() + genh, 3344 name_suffix: 'fa', 3345 dependencies: chardev_ss.dependencies(), 3346 build_by_default: false) 3347 3348chardev = declare_dependency(link_whole: libchardev) 3349 3350hwcore_ss = hwcore_ss.apply(config_host, strict: false) 3351libhwcore = static_library('hwcore', sources: hwcore_ss.sources() + genh, 3352 name_suffix: 'fa', 3353 build_by_default: false) 3354hwcore = declare_dependency(link_whole: libhwcore) 3355common_ss.add(hwcore) 3356 3357########### 3358# Targets # 3359########### 3360 3361emulator_modules = [] 3362foreach m : block_mods + softmmu_mods 3363 emulator_modules += shared_module(m.name(), 3364 build_by_default: true, 3365 name_prefix: '', 3366 link_whole: m, 3367 install: true, 3368 install_dir: qemu_moddir) 3369endforeach 3370if emulator_modules.length() > 0 3371 alias_target('modules', emulator_modules) 3372endif 3373 3374softmmu_ss.add(authz, blockdev, chardev, crypto, io, qmp) 3375common_ss.add(qom, qemuutil) 3376 3377common_ss.add_all(when: 'CONFIG_SOFTMMU', if_true: [softmmu_ss]) 3378common_ss.add_all(when: 'CONFIG_USER_ONLY', if_true: user_ss) 3379 3380common_all = common_ss.apply(config_all, strict: false) 3381common_all = static_library('common', 3382 build_by_default: false, 3383 sources: common_all.sources() + genh, 3384 include_directories: common_user_inc, 3385 implicit_include_directories: false, 3386 dependencies: common_all.dependencies(), 3387 name_suffix: 'fa') 3388 3389feature_to_c = find_program('scripts/feature_to_c.sh') 3390 3391if targetos == 'darwin' 3392 entitlement = find_program('scripts/entitlement.sh') 3393endif 3394 3395emulators = {} 3396foreach target : target_dirs 3397 config_target = config_target_mak[target] 3398 target_name = config_target['TARGET_NAME'] 3399 target_base_arch = config_target['TARGET_BASE_ARCH'] 3400 arch_srcs = [config_target_h[target]] 3401 arch_deps = [] 3402 c_args = ['-DNEED_CPU_H', 3403 '-DCONFIG_TARGET="@0@-config-target.h"'.format(target), 3404 '-DCONFIG_DEVICES="@0@-config-devices.h"'.format(target)] 3405 link_args = emulator_link_args 3406 3407 config_target += config_host 3408 target_inc = [include_directories('target' / config_target['TARGET_BASE_ARCH'])] 3409 if targetos == 'linux' 3410 target_inc += include_directories('linux-headers', is_system: true) 3411 endif 3412 if target.endswith('-softmmu') 3413 target_type='system' 3414 t = target_softmmu_arch[target_base_arch].apply(config_target, strict: false) 3415 arch_srcs += t.sources() 3416 arch_deps += t.dependencies() 3417 3418 hw_dir = target_name == 'sparc64' ? 'sparc64' : target_base_arch 3419 hw = hw_arch[hw_dir].apply(config_target, strict: false) 3420 arch_srcs += hw.sources() 3421 arch_deps += hw.dependencies() 3422 3423 arch_srcs += config_devices_h[target] 3424 link_args += ['@block.syms', '@qemu.syms'] 3425 else 3426 abi = config_target['TARGET_ABI_DIR'] 3427 target_type='user' 3428 target_inc += common_user_inc 3429 if target_base_arch in target_user_arch 3430 t = target_user_arch[target_base_arch].apply(config_target, strict: false) 3431 arch_srcs += t.sources() 3432 arch_deps += t.dependencies() 3433 endif 3434 if 'CONFIG_LINUX_USER' in config_target 3435 base_dir = 'linux-user' 3436 endif 3437 if 'CONFIG_BSD_USER' in config_target 3438 base_dir = 'bsd-user' 3439 target_inc += include_directories('bsd-user/' / targetos) 3440 target_inc += include_directories('bsd-user/host/' / host_arch) 3441 dir = base_dir / abi 3442 arch_srcs += files(dir / 'signal.c', dir / 'target_arch_cpu.c') 3443 endif 3444 target_inc += include_directories( 3445 base_dir, 3446 base_dir / abi, 3447 ) 3448 if 'CONFIG_LINUX_USER' in config_target 3449 dir = base_dir / abi 3450 arch_srcs += files(dir / 'signal.c', dir / 'cpu_loop.c') 3451 if config_target.has_key('TARGET_SYSTBL_ABI') 3452 arch_srcs += \ 3453 syscall_nr_generators[abi].process(base_dir / abi / config_target['TARGET_SYSTBL'], 3454 extra_args : config_target['TARGET_SYSTBL_ABI']) 3455 endif 3456 endif 3457 endif 3458 3459 if 'TARGET_XML_FILES' in config_target 3460 gdbstub_xml = custom_target(target + '-gdbstub-xml.c', 3461 output: target + '-gdbstub-xml.c', 3462 input: files(config_target['TARGET_XML_FILES'].split()), 3463 command: [feature_to_c, '@INPUT@'], 3464 capture: true) 3465 arch_srcs += gdbstub_xml 3466 endif 3467 3468 t = target_arch[target_base_arch].apply(config_target, strict: false) 3469 arch_srcs += t.sources() 3470 arch_deps += t.dependencies() 3471 3472 target_common = common_ss.apply(config_target, strict: false) 3473 objects = common_all.extract_objects(target_common.sources()) 3474 deps = target_common.dependencies() 3475 3476 target_specific = specific_ss.apply(config_target, strict: false) 3477 arch_srcs += target_specific.sources() 3478 arch_deps += target_specific.dependencies() 3479 3480 lib = static_library('qemu-' + target, 3481 sources: arch_srcs + genh, 3482 dependencies: arch_deps, 3483 objects: objects, 3484 include_directories: target_inc, 3485 c_args: c_args, 3486 build_by_default: false, 3487 name_suffix: 'fa') 3488 3489 if target.endswith('-softmmu') 3490 execs = [{ 3491 'name': 'qemu-system-' + target_name, 3492 'win_subsystem': 'console', 3493 'sources': files('softmmu/main.c'), 3494 'dependencies': [] 3495 }] 3496 if targetos == 'windows' and (sdl.found() or gtk.found()) 3497 execs += [{ 3498 'name': 'qemu-system-' + target_name + 'w', 3499 'win_subsystem': 'windows', 3500 'sources': files('softmmu/main.c'), 3501 'dependencies': [] 3502 }] 3503 endif 3504 if get_option('fuzzing') 3505 specific_fuzz = specific_fuzz_ss.apply(config_target, strict: false) 3506 execs += [{ 3507 'name': 'qemu-fuzz-' + target_name, 3508 'win_subsystem': 'console', 3509 'sources': specific_fuzz.sources(), 3510 'dependencies': specific_fuzz.dependencies(), 3511 }] 3512 endif 3513 else 3514 execs = [{ 3515 'name': 'qemu-' + target_name, 3516 'win_subsystem': 'console', 3517 'sources': [], 3518 'dependencies': [] 3519 }] 3520 endif 3521 foreach exe: execs 3522 exe_name = exe['name'] 3523 if targetos == 'darwin' 3524 exe_name += '-unsigned' 3525 endif 3526 3527 emulator = executable(exe_name, exe['sources'], 3528 install: true, 3529 c_args: c_args, 3530 dependencies: arch_deps + deps + exe['dependencies'], 3531 objects: lib.extract_all_objects(recursive: true), 3532 link_language: link_language, 3533 link_depends: [block_syms, qemu_syms] + exe.get('link_depends', []), 3534 link_args: link_args, 3535 win_subsystem: exe['win_subsystem']) 3536 3537 if targetos == 'darwin' 3538 icon = 'pc-bios/qemu.rsrc' 3539 build_input = [emulator, files(icon)] 3540 install_input = [ 3541 get_option('bindir') / exe_name, 3542 meson.current_source_dir() / icon 3543 ] 3544 if 'CONFIG_HVF' in config_target 3545 entitlements = 'accel/hvf/entitlements.plist' 3546 build_input += files(entitlements) 3547 install_input += meson.current_source_dir() / entitlements 3548 endif 3549 3550 emulators += {exe['name'] : custom_target(exe['name'], 3551 input: build_input, 3552 output: exe['name'], 3553 command: [entitlement, '@OUTPUT@', '@INPUT@']) 3554 } 3555 3556 meson.add_install_script(entitlement, '--install', 3557 get_option('bindir') / exe['name'], 3558 install_input) 3559 else 3560 emulators += {exe['name']: emulator} 3561 endif 3562 3563 if stap.found() 3564 foreach stp: [ 3565 {'ext': '.stp-build', 'fmt': 'stap', 'bin': meson.current_build_dir() / exe['name'], 'install': false}, 3566 {'ext': '.stp', 'fmt': 'stap', 'bin': get_option('prefix') / get_option('bindir') / exe['name'], 'install': true}, 3567 {'ext': '-simpletrace.stp', 'fmt': 'simpletrace-stap', 'bin': '', 'install': true}, 3568 {'ext': '-log.stp', 'fmt': 'log-stap', 'bin': '', 'install': true}, 3569 ] 3570 custom_target(exe['name'] + stp['ext'], 3571 input: trace_events_all, 3572 output: exe['name'] + stp['ext'], 3573 install: stp['install'], 3574 install_dir: get_option('datadir') / 'systemtap/tapset', 3575 command: [ 3576 tracetool, '--group=all', '--format=' + stp['fmt'], 3577 '--binary=' + stp['bin'], 3578 '--target-name=' + target_name, 3579 '--target-type=' + target_type, 3580 '--probe-prefix=qemu.' + target_type + '.' + target_name, 3581 '@INPUT@', '@OUTPUT@' 3582 ], 3583 depend_files: tracetool_depends) 3584 endforeach 3585 endif 3586 endforeach 3587endforeach 3588 3589# Other build targets 3590 3591if 'CONFIG_PLUGIN' in config_host 3592 install_headers('include/qemu/qemu-plugin.h') 3593endif 3594 3595subdir('qga') 3596 3597# Don't build qemu-keymap if xkbcommon is not explicitly enabled 3598# when we don't build tools or system 3599if xkbcommon.found() 3600 # used for the update-keymaps target, so include rules even if !have_tools 3601 qemu_keymap = executable('qemu-keymap', files('qemu-keymap.c', 'ui/input-keymap.c') + genh, 3602 dependencies: [qemuutil, xkbcommon], install: have_tools) 3603endif 3604 3605if have_tools 3606 qemu_img = executable('qemu-img', [files('qemu-img.c'), hxdep], 3607 dependencies: [authz, block, crypto, io, qom, qemuutil], install: true) 3608 qemu_io = executable('qemu-io', files('qemu-io.c'), 3609 dependencies: [block, qemuutil], install: true) 3610 qemu_nbd = executable('qemu-nbd', files('qemu-nbd.c'), 3611 dependencies: [blockdev, qemuutil, gnutls, selinux], 3612 install: true) 3613 3614 subdir('storage-daemon') 3615 subdir('contrib/rdmacm-mux') 3616 subdir('contrib/elf2dmp') 3617 3618 executable('qemu-edid', files('qemu-edid.c', 'hw/display/edid-generate.c'), 3619 dependencies: qemuutil, 3620 install: true) 3621 3622 if have_vhost_user 3623 subdir('contrib/vhost-user-blk') 3624 subdir('contrib/vhost-user-gpu') 3625 subdir('contrib/vhost-user-input') 3626 subdir('contrib/vhost-user-scsi') 3627 endif 3628 3629 if targetos == 'linux' 3630 executable('qemu-bridge-helper', files('qemu-bridge-helper.c'), 3631 dependencies: [qemuutil, libcap_ng], 3632 install: true, 3633 install_dir: get_option('libexecdir')) 3634 3635 executable('qemu-pr-helper', files('scsi/qemu-pr-helper.c', 'scsi/utils.c'), 3636 dependencies: [authz, crypto, io, qom, qemuutil, 3637 libcap_ng, mpathpersist], 3638 install: true) 3639 endif 3640 3641 if have_ivshmem 3642 subdir('contrib/ivshmem-client') 3643 subdir('contrib/ivshmem-server') 3644 endif 3645endif 3646 3647subdir('scripts') 3648subdir('tools') 3649subdir('pc-bios') 3650subdir('docs') 3651subdir('tests') 3652if gtk.found() 3653 subdir('po') 3654endif 3655 3656if host_machine.system() == 'windows' 3657 nsis_cmd = [ 3658 find_program('scripts/nsis.py'), 3659 '@OUTPUT@', 3660 get_option('prefix'), 3661 meson.current_source_dir(), 3662 config_host['GLIB_BINDIR'], 3663 host_machine.cpu(), 3664 '--', 3665 '-DDISPLAYVERSION=' + meson.project_version(), 3666 ] 3667 if build_docs 3668 nsis_cmd += '-DCONFIG_DOCUMENTATION=y' 3669 endif 3670 if gtk.found() 3671 nsis_cmd += '-DCONFIG_GTK=y' 3672 endif 3673 3674 nsis = custom_target('nsis', 3675 output: 'qemu-setup-' + meson.project_version() + '.exe', 3676 input: files('qemu.nsi'), 3677 build_always_stale: true, 3678 command: nsis_cmd + ['@INPUT@']) 3679 alias_target('installer', nsis) 3680endif 3681 3682######################### 3683# Configuration summary # 3684######################### 3685 3686# Directories 3687summary_info = {} 3688summary_info += {'Install prefix': get_option('prefix')} 3689summary_info += {'BIOS directory': qemu_datadir} 3690pathsep = targetos == 'windows' ? ';' : ':' 3691summary_info += {'firmware path': pathsep.join(get_option('qemu_firmwarepath'))} 3692summary_info += {'binary directory': get_option('prefix') / get_option('bindir')} 3693summary_info += {'library directory': get_option('prefix') / get_option('libdir')} 3694summary_info += {'module directory': qemu_moddir} 3695summary_info += {'libexec directory': get_option('prefix') / get_option('libexecdir')} 3696summary_info += {'include directory': get_option('prefix') / get_option('includedir')} 3697summary_info += {'config directory': get_option('prefix') / get_option('sysconfdir')} 3698if targetos != 'windows' 3699 summary_info += {'local state directory': get_option('prefix') / get_option('localstatedir')} 3700 summary_info += {'Manual directory': get_option('prefix') / get_option('mandir')} 3701else 3702 summary_info += {'local state directory': 'queried at runtime'} 3703endif 3704summary_info += {'Doc directory': get_option('prefix') / get_option('docdir')} 3705summary_info += {'Build directory': meson.current_build_dir()} 3706summary_info += {'Source path': meson.current_source_dir()} 3707summary_info += {'GIT submodules': config_host['GIT_SUBMODULES']} 3708summary(summary_info, bool_yn: true, section: 'Directories') 3709 3710# Host binaries 3711summary_info = {} 3712summary_info += {'git': config_host['GIT']} 3713summary_info += {'make': config_host['MAKE']} 3714summary_info += {'python': '@0@ (version: @1@)'.format(python.full_path(), python.language_version())} 3715summary_info += {'sphinx-build': sphinx_build} 3716if config_host.has_key('HAVE_GDB_BIN') 3717 summary_info += {'gdb': config_host['HAVE_GDB_BIN']} 3718endif 3719summary_info += {'iasl': iasl} 3720summary_info += {'genisoimage': config_host['GENISOIMAGE']} 3721if targetos == 'windows' and have_ga 3722 summary_info += {'wixl': wixl} 3723endif 3724if slirp.found() and have_system 3725 summary_info += {'smbd': have_slirp_smbd ? smbd_path : false} 3726endif 3727summary(summary_info, bool_yn: true, section: 'Host binaries') 3728 3729# Configurable features 3730summary_info = {} 3731summary_info += {'Documentation': build_docs} 3732summary_info += {'system-mode emulation': have_system} 3733summary_info += {'user-mode emulation': have_user} 3734summary_info += {'block layer': have_block} 3735summary_info += {'Install blobs': get_option('install_blobs')} 3736summary_info += {'module support': config_host.has_key('CONFIG_MODULES')} 3737if config_host.has_key('CONFIG_MODULES') 3738 summary_info += {'alternative module path': get_option('module_upgrades')} 3739endif 3740summary_info += {'fuzzing support': get_option('fuzzing')} 3741if have_system 3742 summary_info += {'Audio drivers': ' '.join(audio_drivers_selected)} 3743endif 3744summary_info += {'Trace backends': ','.join(get_option('trace_backends'))} 3745if 'simple' in get_option('trace_backends') 3746 summary_info += {'Trace output file': get_option('trace_file') + '-<pid>'} 3747endif 3748summary_info += {'D-Bus display': dbus_display} 3749summary_info += {'QOM debugging': get_option('qom_cast_debug')} 3750summary_info += {'vhost-kernel support': have_vhost_kernel} 3751summary_info += {'vhost-net support': have_vhost_net} 3752summary_info += {'vhost-user support': have_vhost_user} 3753summary_info += {'vhost-user-crypto support': have_vhost_user_crypto} 3754summary_info += {'vhost-user-blk server support': have_vhost_user_blk_server} 3755summary_info += {'vhost-vdpa support': have_vhost_vdpa} 3756summary_info += {'build guest agent': have_ga} 3757summary(summary_info, bool_yn: true, section: 'Configurable features') 3758 3759# Compilation information 3760summary_info = {} 3761summary_info += {'host CPU': cpu} 3762summary_info += {'host endianness': build_machine.endian()} 3763summary_info += {'C compiler': ' '.join(meson.get_compiler('c').cmd_array())} 3764summary_info += {'Host C compiler': ' '.join(meson.get_compiler('c', native: true).cmd_array())} 3765if link_language == 'cpp' 3766 summary_info += {'C++ compiler': ' '.join(meson.get_compiler('cpp').cmd_array())} 3767else 3768 summary_info += {'C++ compiler': false} 3769endif 3770if targetos == 'darwin' 3771 summary_info += {'Objective-C compiler': ' '.join(meson.get_compiler('objc').cmd_array())} 3772endif 3773option_cflags = (get_option('debug') ? ['-g'] : []) 3774if get_option('optimization') != 'plain' 3775 option_cflags += ['-O' + get_option('optimization')] 3776endif 3777summary_info += {'CFLAGS': ' '.join(get_option('c_args') + option_cflags)} 3778if link_language == 'cpp' 3779 summary_info += {'CXXFLAGS': ' '.join(get_option('cpp_args') + option_cflags)} 3780endif 3781if targetos == 'darwin' 3782 summary_info += {'OBJCFLAGS': ' '.join(get_option('objc_args') + option_cflags)} 3783endif 3784link_args = get_option(link_language + '_link_args') 3785if link_args.length() > 0 3786 summary_info += {'LDFLAGS': ' '.join(link_args)} 3787endif 3788summary_info += {'QEMU_CFLAGS': ' '.join(qemu_cflags)} 3789if 'cpp' in all_languages 3790 summary_info += {'QEMU_CXXFLAGS': ' '.join(qemu_cxxflags)} 3791endif 3792if 'objc' in all_languages 3793 summary_info += {'QEMU_OBJCFLAGS': ' '.join(qemu_objcflags)} 3794endif 3795summary_info += {'QEMU_LDFLAGS': ' '.join(qemu_ldflags)} 3796summary_info += {'profiler': get_option('profiler')} 3797summary_info += {'link-time optimization (LTO)': get_option('b_lto')} 3798summary_info += {'PIE': get_option('b_pie')} 3799summary_info += {'static build': config_host.has_key('CONFIG_STATIC')} 3800summary_info += {'malloc trim support': has_malloc_trim} 3801summary_info += {'membarrier': have_membarrier} 3802summary_info += {'debug stack usage': get_option('debug_stack_usage')} 3803summary_info += {'mutex debugging': get_option('debug_mutex')} 3804summary_info += {'memory allocator': get_option('malloc')} 3805summary_info += {'avx2 optimization': config_host_data.get('CONFIG_AVX2_OPT')} 3806summary_info += {'avx512bw optimization': config_host_data.get('CONFIG_AVX512BW_OPT')} 3807summary_info += {'avx512f optimization': config_host_data.get('CONFIG_AVX512F_OPT')} 3808if get_option('gprof') 3809 gprof_info = 'YES (deprecated)' 3810else 3811 gprof_info = get_option('gprof') 3812endif 3813summary_info += {'gprof': gprof_info} 3814summary_info += {'gcov': get_option('b_coverage')} 3815summary_info += {'thread sanitizer': config_host.has_key('CONFIG_TSAN')} 3816summary_info += {'CFI support': get_option('cfi')} 3817if get_option('cfi') 3818 summary_info += {'CFI debug support': get_option('cfi_debug')} 3819endif 3820summary_info += {'strip binaries': get_option('strip')} 3821summary_info += {'sparse': sparse} 3822summary_info += {'mingw32 support': targetos == 'windows'} 3823summary(summary_info, bool_yn: true, section: 'Compilation') 3824 3825# snarf the cross-compilation information for tests 3826summary_info = {} 3827have_cross = false 3828foreach target: target_dirs 3829 tcg_mak = meson.current_build_dir() / 'tests/tcg' / target / 'config-target.mak' 3830 if fs.exists(tcg_mak) 3831 config_cross_tcg = keyval.load(tcg_mak) 3832 if 'CC' in config_cross_tcg 3833 summary_info += {config_cross_tcg['TARGET_NAME']: config_cross_tcg['CC']} 3834 have_cross = true 3835 endif 3836 endif 3837endforeach 3838if have_cross 3839 summary(summary_info, bool_yn: true, section: 'Cross compilers') 3840endif 3841 3842# Targets and accelerators 3843summary_info = {} 3844if have_system 3845 summary_info += {'KVM support': config_all.has_key('CONFIG_KVM')} 3846 summary_info += {'HAX support': config_all.has_key('CONFIG_HAX')} 3847 summary_info += {'HVF support': config_all.has_key('CONFIG_HVF')} 3848 summary_info += {'WHPX support': config_all.has_key('CONFIG_WHPX')} 3849 summary_info += {'NVMM support': config_all.has_key('CONFIG_NVMM')} 3850 summary_info += {'Xen support': xen.found()} 3851 if xen.found() 3852 summary_info += {'xen ctrl version': xen.version()} 3853 endif 3854endif 3855summary_info += {'TCG support': config_all.has_key('CONFIG_TCG')} 3856if config_all.has_key('CONFIG_TCG') 3857 if get_option('tcg_interpreter') 3858 summary_info += {'TCG backend': 'TCI (TCG with bytecode interpreter, slow)'} 3859 else 3860 summary_info += {'TCG backend': 'native (@0@)'.format(cpu)} 3861 endif 3862 summary_info += {'TCG plugins': config_host.has_key('CONFIG_PLUGIN')} 3863 summary_info += {'TCG debug enabled': config_host.has_key('CONFIG_DEBUG_TCG')} 3864endif 3865summary_info += {'target list': ' '.join(target_dirs)} 3866if have_system 3867 summary_info += {'default devices': get_option('default_devices')} 3868 summary_info += {'out of process emulation': multiprocess_allowed} 3869 summary_info += {'vfio-user server': vfio_user_server_allowed} 3870endif 3871summary(summary_info, bool_yn: true, section: 'Targets and accelerators') 3872 3873# Block layer 3874summary_info = {} 3875summary_info += {'coroutine backend': config_host['CONFIG_COROUTINE_BACKEND']} 3876summary_info += {'coroutine pool': have_coroutine_pool} 3877if have_block 3878 summary_info += {'Block whitelist (rw)': get_option('block_drv_rw_whitelist')} 3879 summary_info += {'Block whitelist (ro)': get_option('block_drv_ro_whitelist')} 3880 summary_info += {'Use block whitelist in tools': get_option('block_drv_whitelist_in_tools')} 3881 summary_info += {'VirtFS support': have_virtfs} 3882 summary_info += {'build virtiofs daemon': have_virtiofsd} 3883 summary_info += {'Live block migration': config_host_data.get('CONFIG_LIVE_BLOCK_MIGRATION')} 3884 summary_info += {'replication support': config_host_data.get('CONFIG_REPLICATION')} 3885 summary_info += {'bochs support': get_option('bochs').allowed()} 3886 summary_info += {'cloop support': get_option('cloop').allowed()} 3887 summary_info += {'dmg support': get_option('dmg').allowed()} 3888 summary_info += {'qcow v1 support': get_option('qcow1').allowed()} 3889 summary_info += {'vdi support': get_option('vdi').allowed()} 3890 summary_info += {'vvfat support': get_option('vvfat').allowed()} 3891 summary_info += {'qed support': get_option('qed').allowed()} 3892 summary_info += {'parallels support': get_option('parallels').allowed()} 3893 summary_info += {'FUSE exports': fuse} 3894 summary_info += {'VDUSE block exports': have_vduse_blk_export} 3895endif 3896summary(summary_info, bool_yn: true, section: 'Block layer support') 3897 3898# Crypto 3899summary_info = {} 3900summary_info += {'TLS priority': get_option('tls_priority')} 3901summary_info += {'GNUTLS support': gnutls} 3902if gnutls.found() 3903 summary_info += {' GNUTLS crypto': gnutls_crypto.found()} 3904endif 3905summary_info += {'libgcrypt': gcrypt} 3906summary_info += {'nettle': nettle} 3907if nettle.found() 3908 summary_info += {' XTS': xts != 'private'} 3909endif 3910summary_info += {'AF_ALG support': have_afalg} 3911summary_info += {'rng-none': get_option('rng_none')} 3912summary_info += {'Linux keyring': have_keyring} 3913summary(summary_info, bool_yn: true, section: 'Crypto') 3914 3915# Libraries 3916summary_info = {} 3917if targetos == 'darwin' 3918 summary_info += {'Cocoa support': cocoa} 3919 summary_info += {'vmnet.framework support': vmnet} 3920endif 3921summary_info += {'SDL support': sdl} 3922summary_info += {'SDL image support': sdl_image} 3923summary_info += {'GTK support': gtk} 3924summary_info += {'pixman': pixman} 3925summary_info += {'VTE support': vte} 3926summary_info += {'slirp support': slirp} 3927summary_info += {'libtasn1': tasn1} 3928summary_info += {'PAM': pam} 3929summary_info += {'iconv support': iconv} 3930summary_info += {'curses support': curses} 3931summary_info += {'virgl support': virgl} 3932summary_info += {'blkio support': blkio} 3933summary_info += {'curl support': curl} 3934summary_info += {'Multipath support': mpathpersist} 3935summary_info += {'PNG support': png} 3936summary_info += {'VNC support': vnc} 3937if vnc.found() 3938 summary_info += {'VNC SASL support': sasl} 3939 summary_info += {'VNC JPEG support': jpeg} 3940endif 3941if targetos not in ['darwin', 'haiku', 'windows'] 3942 summary_info += {'OSS support': oss} 3943 summary_info += {'sndio support': sndio} 3944elif targetos == 'darwin' 3945 summary_info += {'CoreAudio support': coreaudio} 3946elif targetos == 'windows' 3947 summary_info += {'DirectSound support': dsound} 3948endif 3949if targetos == 'linux' 3950 summary_info += {'ALSA support': alsa} 3951 summary_info += {'PulseAudio support': pulse} 3952endif 3953summary_info += {'JACK support': jack} 3954summary_info += {'brlapi support': brlapi} 3955summary_info += {'vde support': vde} 3956summary_info += {'netmap support': have_netmap} 3957summary_info += {'l2tpv3 support': have_l2tpv3} 3958summary_info += {'Linux AIO support': libaio} 3959summary_info += {'Linux io_uring support': linux_io_uring} 3960summary_info += {'ATTR/XATTR support': libattr} 3961summary_info += {'RDMA support': rdma} 3962summary_info += {'PVRDMA support': have_pvrdma} 3963summary_info += {'fdt support': fdt_opt == 'disabled' ? false : fdt_opt} 3964summary_info += {'libcap-ng support': libcap_ng} 3965summary_info += {'bpf support': libbpf} 3966summary_info += {'spice protocol support': spice_protocol} 3967if spice_protocol.found() 3968 summary_info += {' spice server support': spice} 3969endif 3970summary_info += {'rbd support': rbd} 3971summary_info += {'smartcard support': cacard} 3972summary_info += {'U2F support': u2f} 3973summary_info += {'libusb': libusb} 3974summary_info += {'usb net redir': usbredir} 3975summary_info += {'OpenGL support (epoxy)': opengl} 3976summary_info += {'GBM': gbm} 3977summary_info += {'libiscsi support': libiscsi} 3978summary_info += {'libnfs support': libnfs} 3979if targetos == 'windows' 3980 if have_ga 3981 summary_info += {'QGA VSS support': have_qga_vss} 3982 endif 3983endif 3984summary_info += {'seccomp support': seccomp} 3985summary_info += {'GlusterFS support': glusterfs} 3986summary_info += {'TPM support': have_tpm} 3987summary_info += {'libssh support': libssh} 3988summary_info += {'lzo support': lzo} 3989summary_info += {'snappy support': snappy} 3990summary_info += {'bzip2 support': libbzip2} 3991summary_info += {'lzfse support': liblzfse} 3992summary_info += {'zstd support': zstd} 3993summary_info += {'NUMA host support': numa} 3994summary_info += {'capstone': capstone} 3995summary_info += {'libpmem support': libpmem} 3996summary_info += {'libdaxctl support': libdaxctl} 3997summary_info += {'libudev': libudev} 3998# Dummy dependency, keep .found() 3999summary_info += {'FUSE lseek': fuse_lseek.found()} 4000summary_info += {'selinux': selinux} 4001summary_info += {'libdw': libdw} 4002summary(summary_info, bool_yn: true, section: 'Dependencies') 4003 4004if not supported_cpus.contains(cpu) 4005 message() 4006 warning('SUPPORT FOR THIS HOST CPU WILL GO AWAY IN FUTURE RELEASES!') 4007 message() 4008 message('CPU host architecture ' + cpu + ' support is not currently maintained.') 4009 message('The QEMU project intends to remove support for this host CPU in') 4010 message('a future release if nobody volunteers to maintain it and to') 4011 message('provide a build host for our continuous integration setup.') 4012 message('configure has succeeded and you can continue to build, but') 4013 message('if you care about QEMU on this platform you should contact') 4014 message('us upstream at qemu-devel@nongnu.org.') 4015endif 4016 4017if not supported_oses.contains(targetos) 4018 message() 4019 warning('WARNING: SUPPORT FOR THIS HOST OS WILL GO AWAY IN FUTURE RELEASES!') 4020 message() 4021 message('Host OS ' + targetos + 'support is not currently maintained.') 4022 message('The QEMU project intends to remove support for this host OS in') 4023 message('a future release if nobody volunteers to maintain it and to') 4024 message('provide a build host for our continuous integration setup.') 4025 message('configure has succeeded and you can continue to build, but') 4026 message('if you care about QEMU on this platform you should contact') 4027 message('us upstream at qemu-devel@nongnu.org.') 4028endif 4029