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