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