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