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