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