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