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