configure

   1 #!/bin/sh
   2 #
   3 # qemu configure script (c) 2003 Fabrice Bellard
   4 #
   5
   6 # Unset some variables known to interfere with behavior of common tools,
   7 # just as autoconf does.
   8 CLICOLOR_FORCE= GREP_OPTIONS=
   9 unset CLICOLOR_FORCE GREP_OPTIONS
  10
  11 # Don't allow CCACHE, if present, to use cached results of compile tests!
  12 export CCACHE_RECACHE=yes
  13
  14 # make source path absolute
  15 source_path=$(cd "$(dirname -- "$0")"; pwd)
  16
  17 if test "$PWD" = "$source_path"
  18 then
  19     echo "Using './build' as the directory for build output"
  20
  21     MARKER=build/auto-created-by-configure
  22
  23     if test -e build
  24     then
  25         if test -f $MARKER
  26         then
  27            rm -rf build
  28         else
  29             echo "ERROR: ./build dir already exists and was not previously created by configure"
  30             exit 1
  31         fi
  32     fi
  33
  34     mkdir build
  35     touch $MARKER
  36
  37     cat > GNUmakefile <<'EOF'
  38 # This file is auto-generated by configure to support in-source tree
  39 # 'make' command invocation
  40
  41 ifeq ($(MAKECMDGOALS),)
  42 recurse: all
  43 endif
  44
  45 .NOTPARALLEL: %
  46 %: force
  47         @echo 'changing dir to build for $(MAKE) "$(MAKECMDGOALS)"...'
  48         @$(MAKE) -C build -f Makefile $(MAKECMDGOALS)
  49         @if test "$(MAKECMDGOALS)" = "distclean" && \
  50             test -e build/auto-created-by-configure ; \
  51         then \
  52             rm -rf build GNUmakefile ; \
  53         fi
  54 force: ;
  55 .PHONY: force
  56 GNUmakefile: ;
  57
  58 EOF
  59     cd build
  60     exec $source_path/configure "$@"
  61 fi
  62
  63 # Temporary directory used for files created while
  64 # configure runs. Since it is in the build directory
  65 # we can safely blow away any previous version of it
  66 # (and we need not jump through hoops to try to delete
  67 # it when configure exits.)
  68 TMPDIR1="config-temp"
  69 rm -rf "${TMPDIR1}"
  70 mkdir -p "${TMPDIR1}"
  71 if [ $? -ne 0 ]; then
  72     echo "ERROR: failed to create temporary directory"
  73     exit 1
  74 fi
  75
  76 TMPB="qemu-conf"
  77 TMPC="${TMPDIR1}/${TMPB}.c"
  78 TMPO="${TMPDIR1}/${TMPB}.o"
  79 TMPCXX="${TMPDIR1}/${TMPB}.cxx"
  80 TMPE="${TMPDIR1}/${TMPB}.exe"
  81 TMPTXT="${TMPDIR1}/${TMPB}.txt"
  82
  83 rm -f config.log
  84
  85 # Print a helpful header at the top of config.log
  86 echo "# QEMU configure log $(date)" >> config.log
  87 printf "# Configured with:" >> config.log
  88 printf " '%s'" "$0" "$@" >> config.log
  89 echo >> config.log
  90 echo "#" >> config.log
  91
  92 print_error() {
  93     (echo
  94     echo "ERROR: $1"
  95     while test -n "$2"; do
  96         echo "       $2"
  97         shift
  98     done
  99     echo) >&2
 100 }
 101
 102 error_exit() {
 103     print_error "$@"
 104     exit 1
 105 }
 106
 107 do_compiler() {
 108     # Run the compiler, capturing its output to the log. First argument
 109     # is compiler binary to execute.
 110     local compiler="$1"
 111     shift
 112     if test -n "$BASH_VERSION"; then eval '
 113         echo >>config.log "
 114 funcs: ${FUNCNAME[*]}
 115 lines: ${BASH_LINENO[*]}"
 116     '; fi
 117     echo $compiler "$@" >> config.log
 118     $compiler "$@" >> config.log 2>&1 || return $?
 119     # Test passed. If this is an --enable-werror build, rerun
 120     # the test with -Werror and bail out if it fails. This
 121     # makes warning-generating-errors in configure test code
 122     # obvious to developers.
 123     if test "$werror" != "yes"; then
 124         return 0
 125     fi
 126     # Don't bother rerunning the compile if we were already using -Werror
 127     case "$*" in
 128         *-Werror*)
 129            return 0
 130         ;;
 131     esac
 132     echo $compiler -Werror "$@" >> config.log
 133     $compiler -Werror "$@" >> config.log 2>&1 && return $?
 134     error_exit "configure test passed without -Werror but failed with -Werror." \
 135         "This is probably a bug in the configure script. The failing command" \
 136         "will be at the bottom of config.log." \
 137         "You can run configure with --disable-werror to bypass this check."
 138 }
 139
 140 do_cc() {
 141     do_compiler "$cc" "$@"
 142 }
 143
 144 do_cxx() {
 145     do_compiler "$cxx" "$@"
 146 }
 147
 148 # Append $2 to the variable named $1, with space separation
 149 add_to() {
 150     eval $1=\${$1:+\"\$$1 \"}\$2
 151 }
 152
 153 update_cxxflags() {
 154     # Set QEMU_CXXFLAGS from QEMU_CFLAGS by filtering out those
 155     # options which some versions of GCC's C++ compiler complain about
 156     # because they only make sense for C programs.
 157     QEMU_CXXFLAGS="$QEMU_CXXFLAGS -D__STDC_LIMIT_MACROS -D__STDC_CONSTANT_MACROS -D__STDC_FORMAT_MACROS"
 158     CONFIGURE_CXXFLAGS=$(echo "$CONFIGURE_CFLAGS" | sed s/-std=gnu99/-std=gnu++11/)
 159     for arg in $QEMU_CFLAGS; do
 160         case $arg in
 161             -Wstrict-prototypes|-Wmissing-prototypes|-Wnested-externs|\
 162             -Wold-style-declaration|-Wold-style-definition|-Wredundant-decls)
 163                 ;;
 164             *)
 165                 QEMU_CXXFLAGS=${QEMU_CXXFLAGS:+$QEMU_CXXFLAGS }$arg
 166                 ;;
 167         esac
 168     done
 169 }
 170
 171 compile_object() {
 172   local_cflags="$1"
 173   do_cc $CFLAGS $CONFIGURE_CFLAGS $QEMU_CFLAGS $local_cflags -c -o $TMPO $TMPC
 174 }
 175
 176 compile_prog() {
 177   local_cflags="$1"
 178   local_ldflags="$2"
 179   do_cc $CFLAGS $CONFIGURE_CFLAGS $QEMU_CFLAGS $local_cflags -o $TMPE $TMPC \
 180       $LDFLAGS $CONFIGURE_LDFLAGS $QEMU_LDFLAGS $local_ldflags
 181 }
 182
 183 # symbolically link $1 to $2.  Portable version of "ln -sf".
 184 symlink() {
 185   rm -rf "$2"
 186   mkdir -p "$(dirname "$2")"
 187   ln -s "$1" "$2"
 188 }
 189
 190 # check whether a command is available to this shell (may be either an
 191 # executable or a builtin)
 192 has() {
 193     type "$1" >/dev/null 2>&1
 194 }
 195
 196 version_ge () {
 197     local_ver1=`echo $1 | tr . ' '`
 198     local_ver2=`echo $2 | tr . ' '`
 199     while true; do
 200         set x $local_ver1
 201         local_first=${2-0}
 202         # 'shift 2' if $2 is set, or 'shift' if $2 is not set
 203         shift ${2:+2}
 204         local_ver1=$*
 205         set x $local_ver2
 206         # the second argument finished, the first must be greater or equal
 207         test $# = 1 && return 0
 208         test $local_first -lt $2 && return 1
 209         test $local_first -gt $2 && return 0
 210         shift ${2:+2}
 211         local_ver2=$*
 212     done
 213 }
 214
 215 have_backend () {
 216     echo "$trace_backends" | grep "$1" >/dev/null
 217 }
 218
 219 glob() {
 220     eval test -z '"${1#'"$2"'}"'
 221 }
 222
 223 ld_has() {
 224     $ld --help 2>/dev/null | grep ".$1" >/dev/null 2>&1
 225 }
 226
 227 if printf %s\\n "$source_path" "$PWD" | grep -q "[[:space:]:]";
 228 then
 229   error_exit "main directory cannot contain spaces nor colons"
 230 fi
 231
 232 # default parameters
 233 cpu=""
 234 iasl="iasl"
 235 interp_prefix="/usr/gnemul/qemu-%M"
 236 static="no"
 237 cross_prefix=""
 238 audio_drv_list=""
 239 block_drv_rw_whitelist=""
 240 block_drv_ro_whitelist=""
 241 host_cc="cc"
 242 audio_win_int=""
 243 libs_qga=""
 244 debug_info="yes"
 245 lto="false"
 246 stack_protector=""
 247 safe_stack=""
 248 use_containers="yes"
 249 gdb_bin=$(command -v "gdb-multiarch" || command -v "gdb")
 250
 251 if test -e "$source_path/.git"
 252 then
 253     git_update=yes
 254     git_submodules="ui/keycodemapdb"
 255     git_submodules="$git_submodules tests/fp/berkeley-testfloat-3"
 256     git_submodules="$git_submodules tests/fp/berkeley-softfloat-3"
 257 else
 258     git_update=no
 259     git_submodules=""
 260
 261     if ! test -f "$source_path/ui/keycodemapdb/README"
 262     then
 263         echo
 264         echo "ERROR: missing file $source_path/ui/keycodemapdb/README"
 265         echo
 266         echo "This is not a GIT checkout but module content appears to"
 267         echo "be missing. Do not use 'git archive' or GitHub download links"
 268         echo "to acquire QEMU source archives. Non-GIT builds are only"
 269         echo "supported with source archives linked from:"
 270         echo
 271         echo "  https://www.qemu.org/download/#source"
 272         echo
 273         echo "Developers working with GIT can use scripts/archive-source.sh"
 274         echo "if they need to create valid source archives."
 275         echo
 276         exit 1
 277     fi
 278 fi
 279 git="git"
 280
 281 # Don't accept a target_list environment variable.
 282 unset target_list
 283 unset target_list_exclude
 284
 285 # Default value for a variable defining feature "foo".
 286 #  * foo="no"  feature will only be used if --enable-foo arg is given
 287 #  * foo=""    feature will be searched for, and if found, will be used
 288 #              unless --disable-foo is given
 289 #  * foo="yes" this value will only be set by --enable-foo flag.
 290 #              feature will searched for,
 291 #              if not found, configure exits with error
 292 #
 293 # Always add --enable-foo and --disable-foo command line args.
 294 # Distributions want to ensure that several features are compiled in, and it
 295 # is impossible without a --enable-foo that exits if a feature is not found.
 296
 297 default_feature=""
 298 # parse CC options second
 299 for opt do
 300   optarg=$(expr "x$opt" : 'x[^=]*=\(.*\)')
 301   case "$opt" in
 302       --without-default-features)
 303           default_feature="no"
 304   ;;
 305   esac
 306 done
 307
 308 brlapi="$default_feature"
 309 curl="$default_feature"
 310 iconv="auto"
 311 curses="auto"
 312 docs="auto"
 313 fdt="auto"
 314 netmap="no"
 315 sdl="auto"
 316 sdl_image="auto"
 317 virtiofsd="auto"
 318 virtfs="$default_feature"
 319 libudev="auto"
 320 mpath="auto"
 321 vnc="enabled"
 322 sparse="auto"
 323 vde="$default_feature"
 324 vnc_sasl="auto"
 325 vnc_jpeg="auto"
 326 vnc_png="auto"
 327 xkbcommon="auto"
 328 xen="$default_feature"
 329 xen_ctrl_version="$default_feature"
 330 xen_pci_passthrough="auto"
 331 linux_aio="$default_feature"
 332 linux_io_uring="$default_feature"
 333 cap_ng="$default_feature"
 334 attr="$default_feature"
 335 libattr="$default_feature"
 336 xfs="$default_feature"
 337 tcg="enabled"
 338 membarrier="$default_feature"
 339 vhost_net="$default_feature"
 340 vhost_crypto="$default_feature"
 341 vhost_scsi="$default_feature"
 342 vhost_vsock="$default_feature"
 343 vhost_user="no"
 344 vhost_user_blk_server="auto"
 345 vhost_user_fs="$default_feature"
 346 kvm="auto"
 347 hax="auto"
 348 hvf="auto"
 349 whpx="auto"
 350 rdma="$default_feature"
 351 pvrdma="$default_feature"
 352 gprof="no"
 353 debug_tcg="no"
 354 debug="no"
 355 sanitizers="no"
 356 tsan="no"
 357 fortify_source="$default_feature"
 358 strip_opt="yes"
 359 tcg_interpreter="no"
 360 bigendian="no"
 361 mingw32="no"
 362 gcov="no"
 363 EXESUF="$default_feature"
 364 HOST_DSOSUF=".so"
 365 modules="no"
 366 module_upgrades="no"
 367 prefix="/usr/local"
 368 qemu_suffix="qemu"
 369 slirp="auto"
 370 oss_lib=""
 371 bsd="no"
 372 linux="no"
 373 solaris="no"
 374 profiler="no"
 375 cocoa="auto"
 376 softmmu="yes"
 377 linux_user="no"
 378 bsd_user="no"
 379 blobs="true"
 380 pkgversion=""
 381 pie=""
 382 qom_cast_debug="yes"
 383 trace_backends="log"
 384 trace_file="trace"
 385 spice="$default_feature"
 386 rbd="$default_feature"
 387 smartcard="$default_feature"
 388 u2f="auto"
 389 libusb="$default_feature"
 390 usb_redir="$default_feature"
 391 opengl="$default_feature"
 392 opengl_dmabuf="no"
 393 cpuid_h="no"
 394 avx2_opt="$default_feature"
 395 capstone="auto"
 396 lzo="$default_feature"
 397 snappy="$default_feature"
 398 bzip2="$default_feature"
 399 lzfse="$default_feature"
 400 zstd="$default_feature"
 401 guest_agent="$default_feature"
 402 guest_agent_with_vss="no"
 403 guest_agent_ntddscsi="no"
 404 guest_agent_msi="$default_feature"
 405 vss_win32_sdk="$default_feature"
 406 win_sdk="no"
 407 want_tools="$default_feature"
 408 libiscsi="$default_feature"
 409 libnfs="$default_feature"
 410 coroutine=""
 411 coroutine_pool="$default_feature"
 412 debug_stack_usage="no"
 413 crypto_afalg="no"
 414 cfi="false"
 415 cfi_debug="false"
 416 seccomp="$default_feature"
 417 glusterfs="$default_feature"
 418 glusterfs_xlator_opt="no"
 419 glusterfs_discard="no"
 420 glusterfs_fallocate="no"
 421 glusterfs_zerofill="no"
 422 glusterfs_ftruncate_has_stat="no"
 423 glusterfs_iocb_has_stat="no"
 424 gtk="$default_feature"
 425 gtk_gl="no"
 426 tls_priority="NORMAL"
 427 gnutls="$default_feature"
 428 nettle="$default_feature"
 429 nettle_xts="no"
 430 gcrypt="$default_feature"
 431 gcrypt_hmac="no"
 432 gcrypt_xts="no"
 433 qemu_private_xts="yes"
 434 auth_pam="$default_feature"
 435 vte="$default_feature"
 436 virglrenderer="$default_feature"
 437 tpm="$default_feature"
 438 libssh="$default_feature"
 439 live_block_migration=${default_feature:-yes}
 440 numa="$default_feature"
 441 tcmalloc="no"
 442 jemalloc="no"
 443 replication=${default_feature:-yes}
 444 bochs=${default_feature:-yes}
 445 cloop=${default_feature:-yes}
 446 dmg=${default_feature:-yes}
 447 qcow1=${default_feature:-yes}
 448 vdi=${default_feature:-yes}
 449 vvfat=${default_feature:-yes}
 450 qed=${default_feature:-yes}
 451 parallels=${default_feature:-yes}
 452 sheepdog="no"
 453 libxml2="$default_feature"
 454 debug_mutex="no"
 455 libpmem="$default_feature"
 456 default_devices="yes"
 457 plugins="no"
 458 fuzzing="no"
 459 rng_none="no"
 460 secret_keyring="$default_feature"
 461 libdaxctl="$default_feature"
 462 meson=""
 463 ninja=""
 464 skip_meson=no
 465 gettext="auto"
 466 fuse="auto"
 467 fuse_lseek="auto"
 468
 469 bogus_os="no"
 470 malloc_trim="auto"
 471
 472 # parse CC options second
 473 for opt do
 474   optarg=$(expr "x$opt" : 'x[^=]*=\(.*\)')
 475   case "$opt" in
 476   --cross-prefix=*) cross_prefix="$optarg"
 477   ;;
 478   --cc=*) CC="$optarg"
 479   ;;
 480   --cxx=*) CXX="$optarg"
 481   ;;
 482   --cpu=*) cpu="$optarg"
 483   ;;
 484   --extra-cflags=*) QEMU_CFLAGS="$QEMU_CFLAGS $optarg"
 485                     QEMU_LDFLAGS="$QEMU_LDFLAGS $optarg"
 486   ;;
 487   --extra-cxxflags=*) QEMU_CXXFLAGS="$QEMU_CXXFLAGS $optarg"
 488   ;;
 489   --extra-ldflags=*) QEMU_LDFLAGS="$QEMU_LDFLAGS $optarg"
 490                      EXTRA_LDFLAGS="$optarg"
 491   ;;
 492   --enable-debug-info) debug_info="yes"
 493   ;;
 494   --disable-debug-info) debug_info="no"
 495   ;;
 496   --cross-cc-*[!a-zA-Z0-9_-]*=*) error_exit "Passed bad --cross-cc-FOO option"
 497   ;;
 498   --cross-cc-cflags-*) cc_arch=${opt#--cross-cc-flags-}; cc_arch=${cc_arch%%=*}
 499                       eval "cross_cc_cflags_${cc_arch}=\$optarg"
 500                       cross_cc_vars="$cross_cc_vars cross_cc_cflags_${cc_arch}"
 501   ;;
 502   --cross-cc-*) cc_arch=${opt#--cross-cc-}; cc_arch=${cc_arch%%=*}
 503                 cc_archs="$cc_archs $cc_arch"
 504                 eval "cross_cc_${cc_arch}=\$optarg"
 505                 cross_cc_vars="$cross_cc_vars cross_cc_${cc_arch}"
 506   ;;
 507   esac
 508 done
 509 # OS specific
 510 # Using uname is really, really broken.  Once we have the right set of checks
 511 # we can eliminate its usage altogether.
 512
 513 # Preferred compiler:
 514 #  ${CC} (if set)
 515 #  ${cross_prefix}gcc (if cross-prefix specified)
 516 #  system compiler
 517 if test -z "${CC}${cross_prefix}"; then
 518   cc="$host_cc"
 519 else
 520   cc="${CC-${cross_prefix}gcc}"
 521 fi
 522
 523 if test -z "${CXX}${cross_prefix}"; then
 524   cxx="c++"
 525 else
 526   cxx="${CXX-${cross_prefix}g++}"
 527 fi
 528
 529 ar="${AR-${cross_prefix}ar}"
 530 as="${AS-${cross_prefix}as}"
 531 ccas="${CCAS-$cc}"
 532 cpp="${CPP-$cc -E}"
 533 objcopy="${OBJCOPY-${cross_prefix}objcopy}"
 534 ld="${LD-${cross_prefix}ld}"
 535 ranlib="${RANLIB-${cross_prefix}ranlib}"
 536 nm="${NM-${cross_prefix}nm}"
 537 strip="${STRIP-${cross_prefix}strip}"
 538 windres="${WINDRES-${cross_prefix}windres}"
 539 pkg_config_exe="${PKG_CONFIG-${cross_prefix}pkg-config}"
 540 query_pkg_config() {
 541     "${pkg_config_exe}" ${QEMU_PKG_CONFIG_FLAGS} "$@"
 542 }
 543 pkg_config=query_pkg_config
 544 sdl2_config="${SDL2_CONFIG-${cross_prefix}sdl2-config}"
 545
 546 # If the user hasn't specified ARFLAGS, default to 'rv', just as make does.
 547 ARFLAGS="${ARFLAGS-rv}"
 548
 549 # default flags for all hosts
 550 # We use -fwrapv to tell the compiler that we require a C dialect where
 551 # left shift of signed integers is well defined and has the expected
 552 # 2s-complement style results. (Both clang and gcc agree that it
 553 # provides these semantics.)
 554 QEMU_CFLAGS="-fno-strict-aliasing -fno-common -fwrapv $QEMU_CFLAGS"
 555 QEMU_CFLAGS="-Wundef -Wwrite-strings -Wmissing-prototypes $QEMU_CFLAGS"
 556 QEMU_CFLAGS="-Wstrict-prototypes -Wredundant-decls $QEMU_CFLAGS"
 557 QEMU_CFLAGS="-D_GNU_SOURCE -D_FILE_OFFSET_BITS=64 -D_LARGEFILE_SOURCE $QEMU_CFLAGS"
 558
 559 # Flags that are needed during configure but later taken care of by Meson
 560 CONFIGURE_CFLAGS="-std=gnu99 -Wall"
 561 CONFIGURE_LDFLAGS=
 562
 563
 564 check_define() {
 565 cat > $TMPC <<EOF
 566 #if !defined($1)
 567 #error $1 not defined
 568 #endif
 569 int main(void) { return 0; }
 570 EOF
 571   compile_object
 572 }
 573
 574 check_include() {
 575 cat > $TMPC <<EOF
 576 #include <$1>
 577 int main(void) { return 0; }
 578 EOF
 579   compile_object
 580 }
 581
 582 write_c_skeleton() {
 583     cat > $TMPC <<EOF
 584 int main(void) { return 0; }
 585 EOF
 586 }
 587
 588 write_c_fuzzer_skeleton() {
 589     cat > $TMPC <<EOF
 590 #include <stdint.h>
 591 #include <sys/types.h>
 592 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size);
 593 int LLVMFuzzerTestOneInput(const uint8_t *Data, size_t Size) { return 0; }
 594 EOF
 595 }
 596
 597 if check_define __linux__ ; then
 598   targetos="Linux"
 599 elif check_define _WIN32 ; then
 600   targetos='MINGW32'
 601 elif check_define __OpenBSD__ ; then
 602   targetos='OpenBSD'
 603 elif check_define __sun__ ; then
 604   targetos='SunOS'
 605 elif check_define __HAIKU__ ; then
 606   targetos='Haiku'
 607 elif check_define __FreeBSD__ ; then
 608   targetos='FreeBSD'
 609 elif check_define __FreeBSD_kernel__ && check_define __GLIBC__; then
 610   targetos='GNU/kFreeBSD'
 611 elif check_define __DragonFly__ ; then
 612   targetos='DragonFly'
 613 elif check_define __NetBSD__; then
 614   targetos='NetBSD'
 615 elif check_define __APPLE__; then
 616   targetos='Darwin'
 617 else
 618   # This is a fatal error, but don't report it yet, because we
 619   # might be going to just print the --help text, or it might
 620   # be the result of a missing compiler.
 621   targetos='bogus'
 622   bogus_os='yes'
 623 fi
 624
 625 # Some host OSes need non-standard checks for which CPU to use.
 626 # Note that these checks are broken for cross-compilation: if you're
 627 # cross-compiling to one of these OSes then you'll need to specify
 628 # the correct CPU with the --cpu option.
 629 case $targetos in
 630 Darwin)
 631   # on Leopard most of the system is 32-bit, so we have to ask the kernel if we can
 632   # run 64-bit userspace code.
 633   # If the user didn't specify a CPU explicitly and the kernel says this is
 634   # 64 bit hw, then assume x86_64. Otherwise fall through to the usual detection code.
 635   if test -z "$cpu" && test "$(sysctl -n hw.optional.x86_64)" = "1"; then
 636     cpu="x86_64"
 637   fi
 638   HOST_DSOSUF=".dylib"
 639   ;;
 640 SunOS)
 641   # $(uname -m) returns i86pc even on an x86_64 box, so default based on isainfo
 642   if test -z "$cpu" && test "$(isainfo -k)" = "amd64"; then
 643     cpu="x86_64"
 644   fi
 645 esac
 646
 647 if test ! -z "$cpu" ; then
 648   # command line argument
 649   :
 650 elif check_define __i386__ ; then
 651   cpu="i386"
 652 elif check_define __x86_64__ ; then
 653   if check_define __ILP32__ ; then
 654     cpu="x32"
 655   else
 656     cpu="x86_64"
 657   fi
 658 elif check_define __sparc__ ; then
 659   if check_define __arch64__ ; then
 660     cpu="sparc64"
 661   else
 662     cpu="sparc"
 663   fi
 664 elif check_define _ARCH_PPC ; then
 665   if check_define _ARCH_PPC64 ; then
 666     if check_define _LITTLE_ENDIAN ; then
 667       cpu="ppc64le"
 668     else
 669       cpu="ppc64"
 670     fi
 671   else
 672     cpu="ppc"
 673   fi
 674 elif check_define __mips__ ; then
 675   cpu="mips"
 676 elif check_define __s390__ ; then
 677   if check_define __s390x__ ; then
 678     cpu="s390x"
 679   else
 680     cpu="s390"
 681   fi
 682 elif check_define __riscv ; then
 683   if check_define _LP64 ; then
 684     cpu="riscv64"
 685   else
 686     cpu="riscv32"
 687   fi
 688 elif check_define __arm__ ; then
 689   cpu="arm"
 690 elif check_define __aarch64__ ; then
 691   cpu="aarch64"
 692 else
 693   cpu=$(uname -m)
 694 fi
 695
 696 ARCH=
 697 # Normalise host CPU name and set ARCH.
 698 # Note that this case should only have supported host CPUs, not guests.
 699 case "$cpu" in
 700   ppc|ppc64|s390x|sparc64|x32|riscv32|riscv64)
 701   ;;
 702   ppc64le)
 703     ARCH="ppc64"
 704   ;;
 705   i386|i486|i586|i686|i86pc|BePC)
 706     cpu="i386"
 707   ;;
 708   x86_64|amd64)
 709     cpu="x86_64"
 710   ;;
 711   armv*b|armv*l|arm)
 712     cpu="arm"
 713   ;;
 714   aarch64)
 715     cpu="aarch64"
 716   ;;
 717   mips*)
 718     cpu="mips"
 719   ;;
 720   sparc|sun4[cdmuv])
 721     cpu="sparc"
 722   ;;
 723   *)
 724     # This will result in either an error or falling back to TCI later
 725     ARCH=unknown
 726   ;;
 727 esac
 728 if test -z "$ARCH"; then
 729   ARCH="$cpu"
 730 fi
 731
 732 # OS specific
 733
 734 case $targetos in
 735 MINGW32*)
 736   mingw32="yes"
 737   audio_possible_drivers="dsound sdl"
 738   if check_include dsound.h; then
 739     audio_drv_list="dsound"
 740   else
 741     audio_drv_list=""
 742   fi
 743   supported_os="yes"
 744   pie="no"
 745 ;;
 746 GNU/kFreeBSD)
 747   bsd="yes"
 748   audio_drv_list="oss try-sdl"
 749   audio_possible_drivers="oss sdl pa"
 750 ;;
 751 FreeBSD)
 752   bsd="yes"
 753   make="${MAKE-gmake}"
 754   audio_drv_list="oss try-sdl"
 755   audio_possible_drivers="oss sdl pa"
 756   # needed for kinfo_getvmmap(3) in libutil.h
 757   netmap=""  # enable netmap autodetect
 758 ;;
 759 DragonFly)
 760   bsd="yes"
 761   make="${MAKE-gmake}"
 762   audio_drv_list="oss try-sdl"
 763   audio_possible_drivers="oss sdl pa"
 764 ;;
 765 NetBSD)
 766   bsd="yes"
 767   make="${MAKE-gmake}"
 768   audio_drv_list="oss try-sdl"
 769   audio_possible_drivers="oss sdl"
 770   oss_lib="-lossaudio"
 771 ;;
 772 OpenBSD)
 773   bsd="yes"
 774   make="${MAKE-gmake}"
 775   audio_drv_list="try-sdl"
 776   audio_possible_drivers="sdl"
 777 ;;
 778 Darwin)
 779   bsd="yes"
 780   darwin="yes"
 781   if [ "$cpu" = "x86_64" ] ; then
 782     QEMU_CFLAGS="-arch x86_64 $QEMU_CFLAGS"
 783     QEMU_LDFLAGS="-arch x86_64 $QEMU_LDFLAGS"
 784   fi
 785   cocoa="enabled"
 786   audio_drv_list="coreaudio try-sdl"
 787   audio_possible_drivers="coreaudio sdl"
 788   QEMU_LDFLAGS="-framework CoreFoundation -framework IOKit $QEMU_LDFLAGS"
 789   # Disable attempts to use ObjectiveC features in os/object.h since they
 790   # won't work when we're compiling with gcc as a C compiler.
 791   QEMU_CFLAGS="-DOS_OBJECT_USE_OBJC=0 $QEMU_CFLAGS"
 792 ;;
 793 SunOS)
 794   solaris="yes"
 795   make="${MAKE-gmake}"
 796   smbd="${SMBD-/usr/sfw/sbin/smbd}"
 797   if test -f /usr/include/sys/soundcard.h ; then
 798     audio_drv_list="oss try-sdl"
 799   fi
 800   audio_possible_drivers="oss sdl"
 801 # needed for CMSG_ macros in sys/socket.h
 802   QEMU_CFLAGS="-D_XOPEN_SOURCE=600 $QEMU_CFLAGS"
 803 # needed for TIOCWIN* defines in termios.h
 804   QEMU_CFLAGS="-D__EXTENSIONS__ $QEMU_CFLAGS"
 805 ;;
 806 Haiku)
 807   haiku="yes"
 808   QEMU_CFLAGS="-DB_USE_POSITIVE_POSIX_ERRORS -D_BSD_SOURCE $QEMU_CFLAGS"
 809 ;;
 810 Linux)
 811   audio_drv_list="try-pa oss"
 812   audio_possible_drivers="oss alsa sdl pa"
 813   linux="yes"
 814   linux_user="yes"
 815   vhost_user=${default_feature:-yes}
 816 ;;
 817 esac
 818
 819 if [ "$bsd" = "yes" ] ; then
 820   if [ "$darwin" != "yes" ] ; then
 821     bsd_user="yes"
 822   fi
 823 fi
 824
 825 : ${make=${MAKE-make}}
 826
 827 # We prefer python 3.x. A bare 'python' is traditionally
 828 # python 2.x, but some distros have it as python 3.x, so
 829 # we check that too
 830 python=
 831 explicit_python=no
 832 for binary in "${PYTHON-python3}" python
 833 do
 834     if has "$binary"
 835     then
 836         python=$(command -v "$binary")
 837         break
 838     fi
 839 done
 840
 841
 842 # Check for ancillary tools used in testing
 843 genisoimage=
 844 for binary in genisoimage mkisofs
 845 do
 846     if has $binary
 847     then
 848         genisoimage=$(command -v "$binary")
 849         break
 850     fi
 851 done
 852
 853 : ${smbd=${SMBD-/usr/sbin/smbd}}
 854
 855 # Default objcc to clang if available, otherwise use CC
 856 if has clang; then
 857   objcc=clang
 858 else
 859   objcc="$cc"
 860 fi
 861
 862 if test "$mingw32" = "yes" ; then
 863   EXESUF=".exe"
 864   HOST_DSOSUF=".dll"
 865   # MinGW needs -mthreads for TLS and macro _MT.
 866   CONFIGURE_CFLAGS="-mthreads $CONFIGURE_CFLAGS"
 867   write_c_skeleton;
 868   prefix="/qemu"
 869   qemu_suffix=""
 870   libs_qga="-lws2_32 -lwinmm -lpowrprof -lwtsapi32 -lwininet -liphlpapi -lnetapi32 $libs_qga"
 871 fi
 872
 873 werror=""
 874
 875 for opt do
 876   optarg=$(expr "x$opt" : 'x[^=]*=\(.*\)')
 877   case "$opt" in
 878   --help|-h) show_help=yes
 879   ;;
 880   --version|-V) exec cat $source_path/VERSION
 881   ;;
 882   --prefix=*) prefix="$optarg"
 883   ;;
 884   --interp-prefix=*) interp_prefix="$optarg"
 885   ;;
 886   --cross-prefix=*)
 887   ;;
 888   --cc=*)
 889   ;;
 890   --host-cc=*) host_cc="$optarg"
 891   ;;
 892   --cxx=*)
 893   ;;
 894   --iasl=*) iasl="$optarg"
 895   ;;
 896   --objcc=*) objcc="$optarg"
 897   ;;
 898   --make=*) make="$optarg"
 899   ;;
 900   --install=*)
 901   ;;
 902   --python=*) python="$optarg" ; explicit_python=yes
 903   ;;
 904   --sphinx-build=*) sphinx_build="$optarg"
 905   ;;
 906   --skip-meson) skip_meson=yes
 907   ;;
 908   --meson=*) meson="$optarg"
 909   ;;
 910   --ninja=*) ninja="$optarg"
 911   ;;
 912   --smbd=*) smbd="$optarg"
 913   ;;
 914   --extra-cflags=*)
 915   ;;
 916   --extra-cxxflags=*)
 917   ;;
 918   --extra-ldflags=*)
 919   ;;
 920   --enable-debug-info)
 921   ;;
 922   --disable-debug-info)
 923   ;;
 924   --cross-cc-*)
 925   ;;
 926   --enable-modules)
 927       modules="yes"
 928   ;;
 929   --disable-modules)
 930       modules="no"
 931   ;;
 932   --disable-module-upgrades) module_upgrades="no"
 933   ;;
 934   --enable-module-upgrades) module_upgrades="yes"
 935   ;;
 936   --cpu=*)
 937   ;;
 938   --target-list=*) target_list="$optarg"
 939                    if test "$target_list_exclude"; then
 940                        error_exit "Can't mix --target-list with --target-list-exclude"
 941                    fi
 942   ;;
 943   --target-list-exclude=*) target_list_exclude="$optarg"
 944                    if test "$target_list"; then
 945                        error_exit "Can't mix --target-list-exclude with --target-list"
 946                    fi
 947   ;;
 948   --enable-trace-backends=*) trace_backends="$optarg"
 949   ;;
 950   # XXX: backwards compatibility
 951   --enable-trace-backend=*) trace_backends="$optarg"
 952   ;;
 953   --with-trace-file=*) trace_file="$optarg"
 954   ;;
 955   --with-default-devices) default_devices="yes"
 956   ;;
 957   --without-default-devices) default_devices="no"
 958   ;;
 959   --without-default-features) # processed above
 960   ;;
 961   --enable-gprof) gprof="yes"
 962   ;;
 963   --enable-gcov) gcov="yes"
 964   ;;
 965   --static)
 966     static="yes"
 967     QEMU_PKG_CONFIG_FLAGS="--static $QEMU_PKG_CONFIG_FLAGS"
 968   ;;
 969   --mandir=*) mandir="$optarg"
 970   ;;
 971   --bindir=*) bindir="$optarg"
 972   ;;
 973   --libdir=*) libdir="$optarg"
 974   ;;
 975   --libexecdir=*) libexecdir="$optarg"
 976   ;;
 977   --includedir=*) includedir="$optarg"
 978   ;;
 979   --datadir=*) datadir="$optarg"
 980   ;;
 981   --with-suffix=*) qemu_suffix="$optarg"
 982   ;;
 983   --docdir=*) docdir="$optarg"
 984   ;;
 985   --localedir=*) localedir="$optarg"
 986   ;;
 987   --sysconfdir=*) sysconfdir="$optarg"
 988   ;;
 989   --localstatedir=*) local_statedir="$optarg"
 990   ;;
 991   --firmwarepath=*) firmwarepath="$optarg"
 992   ;;
 993   --host=*|--build=*|\
 994   --disable-dependency-tracking|\
 995   --sbindir=*|--sharedstatedir=*|\
 996   --oldincludedir=*|--datarootdir=*|--infodir=*|\
 997   --htmldir=*|--dvidir=*|--pdfdir=*|--psdir=*)
 998     # These switches are silently ignored, for compatibility with
 999     # autoconf-generated configure scripts. This allows QEMU's
1000     # configure to be used by RPM and similar macros that set
1001     # lots of directory switches by default.
1002   ;;
1003   --disable-sdl) sdl="disabled"
1004   ;;
1005   --enable-sdl) sdl="enabled"
1006   ;;
1007   --disable-sdl-image) sdl_image="disabled"
1008   ;;
1009   --enable-sdl-image) sdl_image="enabled"
1010   ;;
1011   --disable-qom-cast-debug) qom_cast_debug="no"
1012   ;;
1013   --enable-qom-cast-debug) qom_cast_debug="yes"
1014   ;;
1015   --disable-virtfs) virtfs="no"
1016   ;;
1017   --enable-virtfs) virtfs="yes"
1018   ;;
1019   --disable-libudev) libudev="disabled"
1020   ;;
1021   --enable-libudev) libudev="enabled"
1022   ;;
1023   --disable-virtiofsd) virtiofsd="disabled"
1024   ;;
1025   --enable-virtiofsd) virtiofsd="enabled"
1026   ;;
1027   --disable-mpath) mpath="disabled"
1028   ;;
1029   --enable-mpath) mpath="enabled"
1030   ;;
1031   --disable-vnc) vnc="disabled"
1032   ;;
1033   --enable-vnc) vnc="enabled"
1034   ;;
1035   --disable-gettext) gettext="disabled"
1036   ;;
1037   --enable-gettext) gettext="enabled"
1038   ;;
1039   --oss-lib=*) oss_lib="$optarg"
1040   ;;
1041   --audio-drv-list=*) audio_drv_list="$optarg"
1042   ;;
1043   --block-drv-rw-whitelist=*|--block-drv-whitelist=*) block_drv_rw_whitelist=$(echo "$optarg" | sed -e 's/,/ /g')
1044   ;;
1045   --block-drv-ro-whitelist=*) block_drv_ro_whitelist=$(echo "$optarg" | sed -e 's/,/ /g')
1046   ;;
1047   --enable-debug-tcg) debug_tcg="yes"
1048   ;;
1049   --disable-debug-tcg) debug_tcg="no"
1050   ;;
1051   --enable-debug)
1052       # Enable debugging options that aren't excessively noisy
1053       debug_tcg="yes"
1054       debug_mutex="yes"
1055       debug="yes"
1056       strip_opt="no"
1057       fortify_source="no"
1058   ;;
1059   --enable-sanitizers) sanitizers="yes"
1060   ;;
1061   --disable-sanitizers) sanitizers="no"
1062   ;;
1063   --enable-tsan) tsan="yes"
1064   ;;
1065   --disable-tsan) tsan="no"
1066   ;;
1067   --enable-sparse) sparse="enabled"
1068   ;;
1069   --disable-sparse) sparse="disabled"
1070   ;;
1071   --disable-strip) strip_opt="no"
1072   ;;
1073   --disable-vnc-sasl) vnc_sasl="disabled"
1074   ;;
1075   --enable-vnc-sasl) vnc_sasl="enabled"
1076   ;;
1077   --disable-vnc-jpeg) vnc_jpeg="disabled"
1078   ;;
1079   --enable-vnc-jpeg) vnc_jpeg="enabled"
1080   ;;
1081   --disable-vnc-png) vnc_png="disabled"
1082   ;;
1083   --enable-vnc-png) vnc_png="enabled"
1084   ;;
1085   --disable-slirp) slirp="disabled"
1086   ;;
1087   --enable-slirp=git) slirp="internal"
1088   ;;
1089   --enable-slirp=system) slirp="system"
1090   ;;
1091   --disable-vde) vde="no"
1092   ;;
1093   --enable-vde) vde="yes"
1094   ;;
1095   --disable-netmap) netmap="no"
1096   ;;
1097   --enable-netmap) netmap="yes"
1098   ;;
1099   --disable-xen) xen="disabled"
1100   ;;
1101   --enable-xen) xen="enabled"
1102   ;;
1103   --disable-xen-pci-passthrough) xen_pci_passthrough="disabled"
1104   ;;
1105   --enable-xen-pci-passthrough) xen_pci_passthrough="enabled"
1106   ;;
1107   --disable-brlapi) brlapi="no"
1108   ;;
1109   --enable-brlapi) brlapi="yes"
1110   ;;
1111   --disable-kvm) kvm="disabled"
1112   ;;
1113   --enable-kvm) kvm="enabled"
1114   ;;
1115   --disable-hax) hax="disabled"
1116   ;;
1117   --enable-hax) hax="enabled"
1118   ;;
1119   --disable-hvf) hvf="disabled"
1120   ;;
1121   --enable-hvf) hvf="enabled"
1122   ;;
1123   --disable-whpx) whpx="disabled"
1124   ;;
1125   --enable-whpx) whpx="enabled"
1126   ;;
1127   --disable-tcg-interpreter) tcg_interpreter="no"
1128   ;;
1129   --enable-tcg-interpreter) tcg_interpreter="yes"
1130   ;;
1131   --disable-cap-ng)  cap_ng="no"
1132   ;;
1133   --enable-cap-ng) cap_ng="yes"
1134   ;;
1135   --disable-tcg) tcg="disabled"
1136   ;;
1137   --enable-tcg) tcg="enabled"
1138   ;;
1139   --disable-malloc-trim) malloc_trim="disabled"
1140   ;;
1141   --enable-malloc-trim) malloc_trim="enabled"
1142   ;;
1143   --disable-spice) spice="no"
1144   ;;
1145   --enable-spice) spice="yes"
1146   ;;
1147   --disable-libiscsi) libiscsi="no"
1148   ;;
1149   --enable-libiscsi) libiscsi="yes"
1150   ;;
1151   --disable-libnfs) libnfs="no"
1152   ;;
1153   --enable-libnfs) libnfs="yes"
1154   ;;
1155   --enable-profiler) profiler="yes"
1156   ;;
1157   --disable-cocoa) cocoa="disabled"
1158   ;;
1159   --enable-cocoa)
1160       cocoa="enabled" ;
1161       audio_drv_list="coreaudio $(echo $audio_drv_list | sed s,coreaudio,,g)"
1162   ;;
1163   --disable-system) softmmu="no"
1164   ;;
1165   --enable-system) softmmu="yes"
1166   ;;
1167   --disable-user)
1168       linux_user="no" ;
1169       bsd_user="no" ;
1170   ;;
1171   --enable-user) ;;
1172   --disable-linux-user) linux_user="no"
1173   ;;
1174   --enable-linux-user) linux_user="yes"
1175   ;;
1176   --disable-bsd-user) bsd_user="no"
1177   ;;
1178   --enable-bsd-user) bsd_user="yes"
1179   ;;
1180   --enable-pie) pie="yes"
1181   ;;
1182   --disable-pie) pie="no"
1183   ;;
1184   --enable-werror) werror="yes"
1185   ;;
1186   --disable-werror) werror="no"
1187   ;;
1188   --enable-lto) lto="true"
1189   ;;
1190   --disable-lto) lto="false"
1191   ;;
1192   --enable-stack-protector) stack_protector="yes"
1193   ;;
1194   --disable-stack-protector) stack_protector="no"
1195   ;;
1196   --enable-safe-stack) safe_stack="yes"
1197   ;;
1198   --disable-safe-stack) safe_stack="no"
1199   ;;
1200   --enable-cfi)
1201       cfi="true";
1202       lto="true";
1203   ;;
1204   --disable-cfi) cfi="false"
1205   ;;
1206   --enable-cfi-debug) cfi_debug="true"
1207   ;;
1208   --disable-cfi-debug) cfi_debug="false"
1209   ;;
1210   --disable-curses) curses="disabled"
1211   ;;
1212   --enable-curses) curses="enabled"
1213   ;;
1214   --disable-iconv) iconv="disabled"
1215   ;;
1216   --enable-iconv) iconv="enabled"
1217   ;;
1218   --disable-curl) curl="no"
1219   ;;
1220   --enable-curl) curl="yes"
1221   ;;
1222   --disable-fdt) fdt="disabled"
1223   ;;
1224   --enable-fdt) fdt="enabled"
1225   ;;
1226   --enable-fdt=git) fdt="internal"
1227   ;;
1228   --enable-fdt=system) fdt="system"
1229   ;;
1230   --disable-linux-aio) linux_aio="no"
1231   ;;
1232   --enable-linux-aio) linux_aio="yes"
1233   ;;
1234   --disable-linux-io-uring) linux_io_uring="no"
1235   ;;
1236   --enable-linux-io-uring) linux_io_uring="yes"
1237   ;;
1238   --disable-attr) attr="no"
1239   ;;
1240   --enable-attr) attr="yes"
1241   ;;
1242   --disable-membarrier) membarrier="no"
1243   ;;
1244   --enable-membarrier) membarrier="yes"
1245   ;;
1246   --disable-blobs) blobs="false"
1247   ;;
1248   --with-pkgversion=*) pkgversion="$optarg"
1249   ;;
1250   --with-coroutine=*) coroutine="$optarg"
1251   ;;
1252   --disable-coroutine-pool) coroutine_pool="no"
1253   ;;
1254   --enable-coroutine-pool) coroutine_pool="yes"
1255   ;;
1256   --enable-debug-stack-usage) debug_stack_usage="yes"
1257   ;;
1258   --enable-crypto-afalg) crypto_afalg="yes"
1259   ;;
1260   --disable-crypto-afalg) crypto_afalg="no"
1261   ;;
1262   --disable-docs) docs="disabled"
1263   ;;
1264   --enable-docs) docs="enabled"
1265   ;;
1266   --disable-vhost-net) vhost_net="no"
1267   ;;
1268   --enable-vhost-net) vhost_net="yes"
1269   ;;
1270   --disable-vhost-crypto) vhost_crypto="no"
1271   ;;
1272   --enable-vhost-crypto) vhost_crypto="yes"
1273   ;;
1274   --disable-vhost-scsi) vhost_scsi="no"
1275   ;;
1276   --enable-vhost-scsi) vhost_scsi="yes"
1277   ;;
1278   --disable-vhost-vsock) vhost_vsock="no"
1279   ;;
1280   --enable-vhost-vsock) vhost_vsock="yes"
1281   ;;
1282   --disable-vhost-user-blk-server) vhost_user_blk_server="disabled"
1283   ;;
1284   --enable-vhost-user-blk-server) vhost_user_blk_server="enabled"
1285   ;;
1286   --disable-vhost-user-fs) vhost_user_fs="no"
1287   ;;
1288   --enable-vhost-user-fs) vhost_user_fs="yes"
1289   ;;
1290   --disable-opengl) opengl="no"
1291   ;;
1292   --enable-opengl) opengl="yes"
1293   ;;
1294   --disable-rbd) rbd="no"
1295   ;;
1296   --enable-rbd) rbd="yes"
1297   ;;
1298   --disable-xfsctl) xfs="no"
1299   ;;
1300   --enable-xfsctl) xfs="yes"
1301   ;;
1302   --disable-smartcard) smartcard="no"
1303   ;;
1304   --enable-smartcard) smartcard="yes"
1305   ;;
1306   --disable-u2f) u2f="disabled"
1307   ;;
1308   --enable-u2f) u2f="enabled"
1309   ;;
1310   --disable-libusb) libusb="no"
1311   ;;
1312   --enable-libusb) libusb="yes"
1313   ;;
1314   --disable-usb-redir) usb_redir="no"
1315   ;;
1316   --enable-usb-redir) usb_redir="yes"
1317   ;;
1318   --disable-zlib-test)
1319   ;;
1320   --disable-lzo) lzo="no"
1321   ;;
1322   --enable-lzo) lzo="yes"
1323   ;;
1324   --disable-snappy) snappy="no"
1325   ;;
1326   --enable-snappy) snappy="yes"
1327   ;;
1328   --disable-bzip2) bzip2="no"
1329   ;;
1330   --enable-bzip2) bzip2="yes"
1331   ;;
1332   --enable-lzfse) lzfse="yes"
1333   ;;
1334   --disable-lzfse) lzfse="no"
1335   ;;
1336   --disable-zstd) zstd="no"
1337   ;;
1338   --enable-zstd) zstd="yes"
1339   ;;
1340   --enable-guest-agent) guest_agent="yes"
1341   ;;
1342   --disable-guest-agent) guest_agent="no"
1343   ;;
1344   --enable-guest-agent-msi) guest_agent_msi="yes"
1345   ;;
1346   --disable-guest-agent-msi) guest_agent_msi="no"
1347   ;;
1348   --with-vss-sdk) vss_win32_sdk=""
1349   ;;
1350   --with-vss-sdk=*) vss_win32_sdk="$optarg"
1351   ;;
1352   --without-vss-sdk) vss_win32_sdk="no"
1353   ;;
1354   --with-win-sdk) win_sdk=""
1355   ;;
1356   --with-win-sdk=*) win_sdk="$optarg"
1357   ;;
1358   --without-win-sdk) win_sdk="no"
1359   ;;
1360   --enable-tools) want_tools="yes"
1361   ;;
1362   --disable-tools) want_tools="no"
1363   ;;
1364   --enable-seccomp) seccomp="yes"
1365   ;;
1366   --disable-seccomp) seccomp="no"
1367   ;;
1368   --disable-glusterfs) glusterfs="no"
1369   ;;
1370   --disable-avx2) avx2_opt="no"
1371   ;;
1372   --enable-avx2) avx2_opt="yes"
1373   ;;
1374   --disable-avx512f) avx512f_opt="no"
1375   ;;
1376   --enable-avx512f) avx512f_opt="yes"
1377   ;;
1378
1379   --enable-glusterfs) glusterfs="yes"
1380   ;;
1381   --disable-virtio-blk-data-plane|--enable-virtio-blk-data-plane)
1382       echo "$0: $opt is obsolete, virtio-blk data-plane is always on" >&2
1383   ;;
1384   --enable-vhdx|--disable-vhdx)
1385       echo "$0: $opt is obsolete, VHDX driver is always built" >&2
1386   ;;
1387   --enable-uuid|--disable-uuid)
1388       echo "$0: $opt is obsolete, UUID support is always built" >&2
1389   ;;
1390   --disable-gtk) gtk="no"
1391   ;;
1392   --enable-gtk) gtk="yes"
1393   ;;
1394   --tls-priority=*) tls_priority="$optarg"
1395   ;;
1396   --disable-gnutls) gnutls="no"
1397   ;;
1398   --enable-gnutls) gnutls="yes"
1399   ;;
1400   --disable-nettle) nettle="no"
1401   ;;
1402   --enable-nettle) nettle="yes"
1403   ;;
1404   --disable-gcrypt) gcrypt="no"
1405   ;;
1406   --enable-gcrypt) gcrypt="yes"
1407   ;;
1408   --disable-auth-pam) auth_pam="no"
1409   ;;
1410   --enable-auth-pam) auth_pam="yes"
1411   ;;
1412   --enable-rdma) rdma="yes"
1413   ;;
1414   --disable-rdma) rdma="no"
1415   ;;
1416   --enable-pvrdma) pvrdma="yes"
1417   ;;
1418   --disable-pvrdma) pvrdma="no"
1419   ;;
1420   --disable-vte) vte="no"
1421   ;;
1422   --enable-vte) vte="yes"
1423   ;;
1424   --disable-virglrenderer) virglrenderer="no"
1425   ;;
1426   --enable-virglrenderer) virglrenderer="yes"
1427   ;;
1428   --disable-tpm) tpm="no"
1429   ;;
1430   --enable-tpm) tpm="yes"
1431   ;;
1432   --disable-libssh) libssh="no"
1433   ;;
1434   --enable-libssh) libssh="yes"
1435   ;;
1436   --disable-live-block-migration) live_block_migration="no"
1437   ;;
1438   --enable-live-block-migration) live_block_migration="yes"
1439   ;;
1440   --disable-numa) numa="no"
1441   ;;
1442   --enable-numa) numa="yes"
1443   ;;
1444   --disable-libxml2) libxml2="no"
1445   ;;
1446   --enable-libxml2) libxml2="yes"
1447   ;;
1448   --disable-tcmalloc) tcmalloc="no"
1449   ;;
1450   --enable-tcmalloc) tcmalloc="yes"
1451   ;;
1452   --disable-jemalloc) jemalloc="no"
1453   ;;
1454   --enable-jemalloc) jemalloc="yes"
1455   ;;
1456   --disable-replication) replication="no"
1457   ;;
1458   --enable-replication) replication="yes"
1459   ;;
1460   --disable-bochs) bochs="no"
1461   ;;
1462   --enable-bochs) bochs="yes"
1463   ;;
1464   --disable-cloop) cloop="no"
1465   ;;
1466   --enable-cloop) cloop="yes"
1467   ;;
1468   --disable-dmg) dmg="no"
1469   ;;
1470   --enable-dmg) dmg="yes"
1471   ;;
1472   --disable-qcow1) qcow1="no"
1473   ;;
1474   --enable-qcow1) qcow1="yes"
1475   ;;
1476   --disable-vdi) vdi="no"
1477   ;;
1478   --enable-vdi) vdi="yes"
1479   ;;
1480   --disable-vvfat) vvfat="no"
1481   ;;
1482   --enable-vvfat) vvfat="yes"
1483   ;;
1484   --disable-qed) qed="no"
1485   ;;
1486   --enable-qed) qed="yes"
1487   ;;
1488   --disable-parallels) parallels="no"
1489   ;;
1490   --enable-parallels) parallels="yes"
1491   ;;
1492   --disable-sheepdog) sheepdog="no"
1493   ;;
1494   --enable-sheepdog) sheepdog="yes"
1495   ;;
1496   --disable-vhost-user) vhost_user="no"
1497   ;;
1498   --enable-vhost-user) vhost_user="yes"
1499   ;;
1500   --disable-vhost-vdpa) vhost_vdpa="no"
1501   ;;
1502   --enable-vhost-vdpa) vhost_vdpa="yes"
1503   ;;
1504   --disable-vhost-kernel) vhost_kernel="no"
1505   ;;
1506   --enable-vhost-kernel) vhost_kernel="yes"
1507   ;;
1508   --disable-capstone) capstone="disabled"
1509   ;;
1510   --enable-capstone) capstone="enabled"
1511   ;;
1512   --enable-capstone=git) capstone="internal"
1513   ;;
1514   --enable-capstone=system) capstone="system"
1515   ;;
1516   --with-git=*) git="$optarg"
1517   ;;
1518   --enable-git-update) git_update=yes
1519   ;;
1520   --disable-git-update) git_update=no
1521   ;;
1522   --enable-debug-mutex) debug_mutex=yes
1523   ;;
1524   --disable-debug-mutex) debug_mutex=no
1525   ;;
1526   --enable-libpmem) libpmem=yes
1527   ;;
1528   --disable-libpmem) libpmem=no
1529   ;;
1530   --enable-xkbcommon) xkbcommon="enabled"
1531   ;;
1532   --disable-xkbcommon) xkbcommon="disabled"
1533   ;;
1534   --enable-plugins) plugins="yes"
1535   ;;
1536   --disable-plugins) plugins="no"
1537   ;;
1538   --enable-containers) use_containers="yes"
1539   ;;
1540   --disable-containers) use_containers="no"
1541   ;;
1542   --enable-fuzzing) fuzzing=yes
1543   ;;
1544   --disable-fuzzing) fuzzing=no
1545   ;;
1546   --gdb=*) gdb_bin="$optarg"
1547   ;;
1548   --enable-rng-none) rng_none=yes
1549   ;;
1550   --disable-rng-none) rng_none=no
1551   ;;
1552   --enable-keyring) secret_keyring="yes"
1553   ;;
1554   --disable-keyring) secret_keyring="no"
1555   ;;
1556   --enable-libdaxctl) libdaxctl=yes
1557   ;;
1558   --disable-libdaxctl) libdaxctl=no
1559   ;;
1560   --enable-fuse) fuse="enabled"
1561   ;;
1562   --disable-fuse) fuse="disabled"
1563   ;;
1564   --enable-fuse-lseek) fuse_lseek="enabled"
1565   ;;
1566   --disable-fuse-lseek) fuse_lseek="disabled"
1567   ;;
1568   *)
1569       echo "ERROR: unknown option $opt"
1570       echo "Try '$0 --help' for more information"
1571       exit 1
1572   ;;
1573   esac
1574 done
1575
1576 libdir="${libdir:-$prefix/lib}"
1577 libexecdir="${libexecdir:-$prefix/libexec}"
1578 includedir="${includedir:-$prefix/include}"
1579
1580 if test "$mingw32" = "yes" ; then
1581     mandir="$prefix"
1582     datadir="$prefix"
1583     docdir="$prefix"
1584     bindir="$prefix"
1585     sysconfdir="$prefix"
1586     local_statedir="$prefix"
1587 else
1588     mandir="${mandir:-$prefix/share/man}"
1589     datadir="${datadir:-$prefix/share}"
1590     docdir="${docdir:-$prefix/share/doc}"
1591     bindir="${bindir:-$prefix/bin}"
1592     sysconfdir="${sysconfdir:-$prefix/etc}"
1593     local_statedir="${local_statedir:-$prefix/var}"
1594 fi
1595 firmwarepath="${firmwarepath:-$datadir/qemu-firmware}"
1596 localedir="${localedir:-$datadir/locale}"
1597
1598 case "$cpu" in
1599     ppc)
1600            CPU_CFLAGS="-m32"
1601            QEMU_LDFLAGS="-m32 $QEMU_LDFLAGS"
1602            ;;
1603     ppc64)
1604            CPU_CFLAGS="-m64"
1605            QEMU_LDFLAGS="-m64 $QEMU_LDFLAGS"
1606            ;;
1607     sparc)
1608            CPU_CFLAGS="-m32 -mv8plus -mcpu=ultrasparc"
1609            QEMU_LDFLAGS="-m32 -mv8plus $QEMU_LDFLAGS"
1610            ;;
1611     sparc64)
1612            CPU_CFLAGS="-m64 -mcpu=ultrasparc"
1613            QEMU_LDFLAGS="-m64 $QEMU_LDFLAGS"
1614            ;;
1615     s390)
1616            CPU_CFLAGS="-m31"
1617            QEMU_LDFLAGS="-m31 $QEMU_LDFLAGS"
1618            ;;
1619     s390x)
1620            CPU_CFLAGS="-m64"
1621            QEMU_LDFLAGS="-m64 $QEMU_LDFLAGS"
1622            ;;
1623     i386)
1624            CPU_CFLAGS="-m32"
1625            QEMU_LDFLAGS="-m32 $QEMU_LDFLAGS"
1626            ;;
1627     x86_64)
1628            # ??? Only extremely old AMD cpus do not have cmpxchg16b.
1629            # If we truly care, we should simply detect this case at
1630            # runtime and generate the fallback to serial emulation.
1631            CPU_CFLAGS="-m64 -mcx16"
1632            QEMU_LDFLAGS="-m64 $QEMU_LDFLAGS"
1633            ;;
1634     x32)
1635            CPU_CFLAGS="-mx32"
1636            QEMU_LDFLAGS="-mx32 $QEMU_LDFLAGS"
1637            ;;
1638     # No special flags required for other host CPUs
1639 esac
1640
1641 eval "cross_cc_${cpu}=\$host_cc"
1642 cross_cc_vars="$cross_cc_vars cross_cc_${cpu}"
1643 QEMU_CFLAGS="$CPU_CFLAGS $QEMU_CFLAGS"
1644
1645 # For user-mode emulation the host arch has to be one we explicitly
1646 # support, even if we're using TCI.
1647 if [ "$ARCH" = "unknown" ]; then
1648   bsd_user="no"
1649   linux_user="no"
1650 fi
1651
1652 default_target_list=""
1653 deprecated_targets_list=ppc64abi32-linux-user,tilegx-linux-user,lm32-softmmu,unicore32-softmmu
1654 deprecated_features=""
1655 mak_wilds=""
1656
1657 if [ "$softmmu" = "yes" ]; then
1658     mak_wilds="${mak_wilds} $source_path/default-configs/targets/*-softmmu.mak"
1659 fi
1660 if [ "$linux_user" = "yes" ]; then
1661     mak_wilds="${mak_wilds} $source_path/default-configs/targets/*-linux-user.mak"
1662 fi
1663 if [ "$bsd_user" = "yes" ]; then
1664     mak_wilds="${mak_wilds} $source_path/default-configs/targets/*-bsd-user.mak"
1665 fi
1666
1667 # If the user doesn't explicitly specify a deprecated target we will
1668 # skip it.
1669 if test -z "$target_list"; then
1670     if test -z "$target_list_exclude"; then
1671         target_list_exclude="$deprecated_targets_list"
1672     else
1673         target_list_exclude="$target_list_exclude,$deprecated_targets_list"
1674     fi
1675 fi
1676
1677 for config in $mak_wilds; do
1678     target="$(basename "$config" .mak)"
1679     if echo "$target_list_exclude" | grep -vq "$target"; then
1680         default_target_list="${default_target_list} $target"
1681     fi
1682 done
1683
1684 # Enumerate public trace backends for --help output
1685 trace_backend_list=$(echo $(grep -le '^PUBLIC = True$' "$source_path"/scripts/tracetool/backend/*.py | sed -e 's/^.*\/\(.*\)\.py$/\1/'))
1686
1687 if test x"$show_help" = x"yes" ; then
1688 cat << EOF
1689
1690 Usage: configure [options]
1691 Options: [defaults in brackets after descriptions]
1692
1693 Standard options:
1694   --help                   print this message
1695   --prefix=PREFIX          install in PREFIX [$prefix]
1696   --interp-prefix=PREFIX   where to find shared libraries, etc.
1697                            use %M for cpu name [$interp_prefix]
1698   --target-list=LIST       set target list (default: build all non-deprecated)
1699 $(echo Available targets: $default_target_list | \
1700   fold -s -w 53 | sed -e 's/^/                           /')
1701 $(echo Deprecated targets: $deprecated_targets_list | \
1702   fold -s -w 53 | sed -e 's/^/                           /')
1703   --target-list-exclude=LIST exclude a set of targets from the default target-list
1704
1705 Advanced options (experts only):
1706   --cross-prefix=PREFIX    use PREFIX for compile tools [$cross_prefix]
1707   --cc=CC                  use C compiler CC [$cc]
1708   --iasl=IASL              use ACPI compiler IASL [$iasl]
1709   --host-cc=CC             use C compiler CC [$host_cc] for code run at
1710                            build time
1711   --cxx=CXX                use C++ compiler CXX [$cxx]
1712   --objcc=OBJCC            use Objective-C compiler OBJCC [$objcc]
1713   --extra-cflags=CFLAGS    append extra C compiler flags QEMU_CFLAGS
1714   --extra-cxxflags=CXXFLAGS append extra C++ compiler flags QEMU_CXXFLAGS
1715   --extra-ldflags=LDFLAGS  append extra linker flags LDFLAGS
1716   --cross-cc-ARCH=CC       use compiler when building ARCH guest test cases
1717   --cross-cc-flags-ARCH=   use compiler flags when building ARCH guest tests
1718   --make=MAKE              use specified make [$make]
1719   --python=PYTHON          use specified python [$python]
1720   --sphinx-build=SPHINX    use specified sphinx-build [$sphinx_build]
1721   --meson=MESON            use specified meson [$meson]
1722   --ninja=NINJA            use specified ninja [$ninja]
1723   --smbd=SMBD              use specified smbd [$smbd]
1724   --with-git=GIT           use specified git [$git]
1725   --static                 enable static build [$static]
1726   --mandir=PATH            install man pages in PATH
1727   --datadir=PATH           install firmware in PATH/$qemu_suffix
1728   --localedir=PATH         install translation in PATH/$qemu_suffix
1729   --docdir=PATH            install documentation in PATH/$qemu_suffix
1730   --bindir=PATH            install binaries in PATH
1731   --libdir=PATH            install libraries in PATH
1732   --libexecdir=PATH        install helper binaries in PATH
1733   --sysconfdir=PATH        install config in PATH/$qemu_suffix
1734   --localstatedir=PATH     install local state in PATH (set at runtime on win32)
1735   --firmwarepath=PATH      search PATH for firmware files
1736   --efi-aarch64=PATH       PATH of efi file to use for aarch64 VMs.
1737   --with-suffix=SUFFIX     suffix for QEMU data inside datadir/libdir/sysconfdir/docdir [$qemu_suffix]
1738   --with-pkgversion=VERS   use specified string as sub-version of the package
1739   --without-default-features default all --enable-* options to "disabled"
1740   --without-default-devices  do not include any device that is not needed to
1741                            start the emulator (only use if you are including
1742                            desired devices in default-configs/devices/)
1743   --enable-debug           enable common debug build options
1744   --enable-sanitizers      enable default sanitizers
1745   --enable-tsan            enable thread sanitizer
1746   --disable-strip          disable stripping binaries
1747   --disable-werror         disable compilation abort on warning
1748   --disable-stack-protector disable compiler-provided stack protection
1749   --audio-drv-list=LIST    set audio drivers list:
1750                            Available drivers: $audio_possible_drivers
1751   --block-drv-whitelist=L  Same as --block-drv-rw-whitelist=L
1752   --block-drv-rw-whitelist=L
1753                            set block driver read-write whitelist
1754                            (affects only QEMU, not qemu-img)
1755   --block-drv-ro-whitelist=L
1756                            set block driver read-only whitelist
1757                            (affects only QEMU, not qemu-img)
1758   --enable-trace-backends=B Set trace backend
1759                            Available backends: $trace_backend_list
1760   --with-trace-file=NAME   Full PATH,NAME of file to store traces
1761                            Default:trace-<pid>
1762   --disable-slirp          disable SLIRP userspace network connectivity
1763   --enable-tcg-interpreter enable TCG with bytecode interpreter (TCI)
1764   --enable-malloc-trim     enable libc malloc_trim() for memory optimization
1765   --oss-lib                path to OSS library
1766   --cpu=CPU                Build for host CPU [$cpu]
1767   --with-coroutine=BACKEND coroutine backend. Supported options:
1768                            ucontext, sigaltstack, windows
1769   --enable-gcov            enable test coverage analysis with gcov
1770   --disable-blobs          disable installing provided firmware blobs
1771   --with-vss-sdk=SDK-path  enable Windows VSS support in QEMU Guest Agent
1772   --with-win-sdk=SDK-path  path to Windows Platform SDK (to build VSS .tlb)
1773   --tls-priority           default TLS protocol/cipher priority string
1774   --enable-gprof           QEMU profiling with gprof
1775   --enable-profiler        profiler support
1776   --enable-debug-stack-usage
1777                            track the maximum stack usage of stacks created by qemu_alloc_stack
1778   --enable-plugins
1779                            enable plugins via shared library loading
1780   --disable-containers     don't use containers for cross-building
1781   --gdb=GDB-path           gdb to use for gdbstub tests [$gdb_bin]
1782
1783 Optional features, enabled with --enable-FEATURE and
1784 disabled with --disable-FEATURE, default is enabled if available
1785 (unless built with --without-default-features):
1786
1787   system          all system emulation targets
1788   user            supported user emulation targets
1789   linux-user      all linux usermode emulation targets
1790   bsd-user        all BSD usermode emulation targets
1791   docs            build documentation
1792   guest-agent     build the QEMU Guest Agent
1793   guest-agent-msi build guest agent Windows MSI installation package
1794   pie             Position Independent Executables
1795   modules         modules support (non-Windows)
1796   module-upgrades try to load modules from alternate paths for upgrades
1797   debug-tcg       TCG debugging (default is disabled)
1798   debug-info      debugging information
1799   lto             Enable Link-Time Optimization.
1800   sparse          sparse checker
1801   safe-stack      SafeStack Stack Smash Protection. Depends on
1802                   clang/llvm >= 3.7 and requires coroutine backend ucontext.
1803   cfi             Enable Control-Flow Integrity for indirect function calls.
1804                   In case of a cfi violation, QEMU is terminated with SIGILL
1805                   Depends on lto and is incompatible with modules
1806                   Automatically enables Link-Time Optimization (lto)
1807   cfi-debug       In case of a cfi violation, a message containing the line that
1808                   triggered the error is written to stderr. After the error,
1809                   QEMU is still terminated with SIGILL
1810   gnutls          GNUTLS cryptography support
1811   nettle          nettle cryptography support
1812   gcrypt          libgcrypt cryptography support
1813   auth-pam        PAM access control
1814   sdl             SDL UI
1815   sdl-image       SDL Image support for icons
1816   gtk             gtk UI
1817   vte             vte support for the gtk UI
1818   curses          curses UI
1819   iconv           font glyph conversion support
1820   vnc             VNC UI support
1821   vnc-sasl        SASL encryption for VNC server
1822   vnc-jpeg        JPEG lossy compression for VNC server
1823   vnc-png         PNG compression for VNC server
1824   cocoa           Cocoa UI (Mac OS X only)
1825   virtfs          VirtFS
1826   virtiofsd       build virtiofs daemon (virtiofsd)
1827   libudev         Use libudev to enumerate host devices
1828   mpath           Multipath persistent reservation passthrough
1829   xen             xen backend driver support
1830   xen-pci-passthrough    PCI passthrough support for Xen
1831   brlapi          BrlAPI (Braile)
1832   curl            curl connectivity
1833   membarrier      membarrier system call (for Linux 4.14+ or Windows)
1834   fdt             fdt device tree
1835   kvm             KVM acceleration support
1836   hax             HAX acceleration support
1837   hvf             Hypervisor.framework acceleration support
1838   whpx            Windows Hypervisor Platform acceleration support
1839   rdma            Enable RDMA-based migration
1840   pvrdma          Enable PVRDMA support
1841   vde             support for vde network
1842   netmap          support for netmap network
1843   linux-aio       Linux AIO support
1844   linux-io-uring  Linux io_uring support
1845   cap-ng          libcap-ng support
1846   attr            attr and xattr support
1847   vhost-net       vhost-net kernel acceleration support
1848   vhost-vsock     virtio sockets device support
1849   vhost-scsi      vhost-scsi kernel target support
1850   vhost-crypto    vhost-user-crypto backend support
1851   vhost-kernel    vhost kernel backend support
1852   vhost-user      vhost-user backend support
1853   vhost-user-blk-server    vhost-user-blk server support
1854   vhost-vdpa      vhost-vdpa kernel backend support
1855   spice           spice
1856   rbd             rados block device (rbd)
1857   libiscsi        iscsi support
1858   libnfs          nfs support
1859   smartcard       smartcard support (libcacard)
1860   u2f             U2F support (u2f-emu)
1861   libusb          libusb (for usb passthrough)
1862   live-block-migration   Block migration in the main migration stream
1863   usb-redir       usb network redirection support
1864   lzo             support of lzo compression library
1865   snappy          support of snappy compression library
1866   bzip2           support of bzip2 compression library
1867                   (for reading bzip2-compressed dmg images)
1868   lzfse           support of lzfse compression library
1869                   (for reading lzfse-compressed dmg images)
1870   zstd            support for zstd compression library
1871                   (for migration compression and qcow2 cluster compression)
1872   seccomp         seccomp support
1873   coroutine-pool  coroutine freelist (better performance)
1874   glusterfs       GlusterFS backend
1875   tpm             TPM support
1876   libssh          ssh block device support
1877   numa            libnuma support
1878   libxml2         for Parallels image format
1879   tcmalloc        tcmalloc support
1880   jemalloc        jemalloc support
1881   avx2            AVX2 optimization support
1882   avx512f         AVX512F optimization support
1883   replication     replication support
1884   opengl          opengl support
1885   virglrenderer   virgl rendering support
1886   xfsctl          xfsctl support
1887   qom-cast-debug  cast debugging support
1888   tools           build qemu-io, qemu-nbd and qemu-img tools
1889   bochs           bochs image format support
1890   cloop           cloop image format support
1891   dmg             dmg image format support
1892   qcow1           qcow v1 image format support
1893   vdi             vdi image format support
1894   vvfat           vvfat image format support
1895   qed             qed image format support
1896   parallels       parallels image format support
1897   sheepdog        sheepdog block driver support (deprecated)
1898   crypto-afalg    Linux AF_ALG crypto backend driver
1899   capstone        capstone disassembler support
1900   debug-mutex     mutex debugging support
1901   libpmem         libpmem support
1902   xkbcommon       xkbcommon support
1903   rng-none        dummy RNG, avoid using /dev/(u)random and getrandom()
1904   libdaxctl       libdaxctl support
1905   fuse            FUSE block device export
1906   fuse-lseek      SEEK_HOLE/SEEK_DATA support for FUSE exports
1907
1908 NOTE: The object files are built at the place where configure is launched
1909 EOF
1910 exit 0
1911 fi
1912
1913 # Remove old dependency files to make sure that they get properly regenerated
1914 rm -f */config-devices.mak.d
1915
1916 if test -z "$python"
1917 then
1918     error_exit "Python not found. Use --python=/path/to/python"
1919 fi
1920 if ! has "$make"
1921 then
1922     error_exit "GNU make ($make) not found"
1923 fi
1924
1925 # Note that if the Python conditional here evaluates True we will exit
1926 # with status 1 which is a shell 'false' value.
1927 if ! $python -c 'import sys; sys.exit(sys.version_info < (3,6))'; then
1928   error_exit "Cannot use '$python', Python >= 3.6 is required." \
1929       "Use --python=/path/to/python to specify a supported Python."
1930 fi
1931
1932 # Preserve python version since some functionality is dependent on it
1933 python_version=$($python -c 'import sys; print("%d.%d.%d" % (sys.version_info[0], sys.version_info[1], sys.version_info[2]))' 2>/dev/null)
1934
1935 # Suppress writing compiled files
1936 python="$python -B"
1937
1938 if test -z "$meson"; then
1939     if test "$explicit_python" = no && has meson && version_ge "$(meson --version)" 0.55.3; then
1940         meson=meson
1941     elif test -e "${source_path}/.git" && test $git_update = 'yes' ; then
1942         meson=git
1943     elif test -e "${source_path}/meson/meson.py" ; then
1944         meson=internal
1945     else
1946         if test "$explicit_python" = yes; then
1947             error_exit "--python requires using QEMU's embedded Meson distribution, but it was not found."
1948         else
1949             error_exit "Meson not found.  Use --meson=/path/to/meson"
1950         fi
1951     fi
1952 else
1953     # Meson uses its own Python interpreter to invoke other Python scripts,
1954     # but the user wants to use the one they specified with --python.
1955     #
1956     # We do not want to override the distro Python interpreter (and sometimes
1957     # cannot: for example in Homebrew /usr/bin/meson is a bash script), so
1958     # just require --meson=git|internal together with --python.
1959     if test "$explicit_python" = yes; then
1960         case "$meson" in
1961             git | internal) ;;
1962             *) error_exit "--python requires using QEMU's embedded Meson distribution." ;;
1963         esac
1964     fi
1965 fi
1966
1967 if test "$meson" = git; then
1968     git_submodules="${git_submodules} meson"
1969 fi
1970
1971 case "$meson" in
1972     git | internal)
1973         meson="$python ${source_path}/meson/meson.py"
1974         ;;
1975     *) meson=$(command -v "$meson") ;;
1976 esac
1977
1978 # Probe for ninja
1979
1980 if test -z "$ninja"; then
1981     for c in ninja ninja-build samu; do
1982         if has $c; then
1983             ninja=$(command -v "$c")
1984             break
1985         fi
1986     done
1987     if test -z "$ninja"; then
1988       error_exit "Cannot find Ninja"
1989     fi
1990 fi
1991
1992 # Check that the C compiler works. Doing this here before testing
1993 # the host CPU ensures that we had a valid CC to autodetect the
1994 # $cpu var (and we should bail right here if that's not the case).
1995 # It also allows the help message to be printed without a CC.
1996 write_c_skeleton;
1997 if compile_object ; then
1998   : C compiler works ok
1999 else
2000     error_exit "\"$cc\" either does not exist or does not work"
2001 fi
2002 if ! compile_prog ; then
2003     error_exit "\"$cc\" cannot build an executable (is your linker broken?)"
2004 fi
2005
2006 # Consult white-list to determine whether to enable werror
2007 # by default.  Only enable by default for git builds
2008 if test -z "$werror" ; then
2009     if test -e "$source_path/.git" && \
2010         { test "$linux" = "yes" || test "$mingw32" = "yes"; }; then
2011         werror="yes"
2012     else
2013         werror="no"
2014     fi
2015 fi
2016
2017 if test "$bogus_os" = "yes"; then
2018     # Now that we know that we're not printing the help and that
2019     # the compiler works (so the results of the check_defines we used
2020     # to identify the OS are reliable), if we didn't recognize the
2021     # host OS we should stop now.
2022     error_exit "Unrecognized host OS (uname -s reports '$(uname -s)')"
2023 fi
2024
2025 # Check whether the compiler matches our minimum requirements:
2026 cat > $TMPC << EOF
2027 #if defined(__clang_major__) && defined(__clang_minor__)
2028 # ifdef __apple_build_version__
2029 #  if __clang_major__ < 5 || (__clang_major__ == 5 && __clang_minor__ < 1)
2030 #   error You need at least XCode Clang v5.1 to compile QEMU
2031 #  endif
2032 # else
2033 #  if __clang_major__ < 3 || (__clang_major__ == 3 && __clang_minor__ < 4)
2034 #   error You need at least Clang v3.4 to compile QEMU
2035 #  endif
2036 # endif
2037 #elif defined(__GNUC__) && defined(__GNUC_MINOR__)
2038 # if __GNUC__ < 4 || (__GNUC__ == 4 && __GNUC_MINOR__ < 8)
2039 #  error You need at least GCC v4.8 to compile QEMU
2040 # endif
2041 #else
2042 # error You either need GCC or Clang to compiler QEMU
2043 #endif
2044 int main (void) { return 0; }
2045 EOF
2046 if ! compile_prog "" "" ; then
2047     error_exit "You need at least GCC v4.8 or Clang v3.4 (or XCode Clang v5.1)"
2048 fi
2049
2050 # Accumulate -Wfoo and -Wno-bar separately.
2051 # We will list all of the enable flags first, and the disable flags second.
2052 # Note that we do not add -Werror, because that would enable it for all
2053 # configure tests. If a configure test failed due to -Werror this would
2054 # just silently disable some features, so it's too error prone.
2055
2056 warn_flags=
2057 add_to warn_flags -Wold-style-declaration
2058 add_to warn_flags -Wold-style-definition
2059 add_to warn_flags -Wtype-limits
2060 add_to warn_flags -Wformat-security
2061 add_to warn_flags -Wformat-y2k
2062 add_to warn_flags -Winit-self
2063 add_to warn_flags -Wignored-qualifiers
2064 add_to warn_flags -Wempty-body
2065 add_to warn_flags -Wnested-externs
2066 add_to warn_flags -Wendif-labels
2067 add_to warn_flags -Wexpansion-to-defined
2068 add_to warn_flags -Wimplicit-fallthrough=2
2069
2070 nowarn_flags=
2071 add_to nowarn_flags -Wno-initializer-overrides
2072 add_to nowarn_flags -Wno-missing-include-dirs
2073 add_to nowarn_flags -Wno-shift-negative-value
2074 add_to nowarn_flags -Wno-string-plus-int
2075 add_to nowarn_flags -Wno-typedef-redefinition
2076 add_to nowarn_flags -Wno-tautological-type-limit-compare
2077 add_to nowarn_flags -Wno-psabi
2078
2079 gcc_flags="$warn_flags $nowarn_flags"
2080
2081 cc_has_warning_flag() {
2082     write_c_skeleton;
2083
2084     # Use the positive sense of the flag when testing for -Wno-wombat
2085     # support (gcc will happily accept the -Wno- form of unknown
2086     # warning options).
2087     optflag="$(echo $1 | sed -e 's/^-Wno-/-W/')"
2088     compile_prog "-Werror $optflag" ""
2089 }
2090
2091 for flag in $gcc_flags; do
2092     if cc_has_warning_flag $flag ; then
2093         QEMU_CFLAGS="$QEMU_CFLAGS $flag"
2094     fi
2095 done
2096
2097 if test "$stack_protector" != "no"; then
2098   cat > $TMPC << EOF
2099 int main(int argc, char *argv[])
2100 {
2101     char arr[64], *p = arr, *c = argv[0];
2102     while (*c) {
2103         *p++ = *c++;
2104     }
2105     return 0;
2106 }
2107 EOF
2108   gcc_flags="-fstack-protector-strong -fstack-protector-all"
2109   sp_on=0
2110   for flag in $gcc_flags; do
2111     # We need to check both a compile and a link, since some compiler
2112     # setups fail only on a .c->.o compile and some only at link time
2113     if compile_object "-Werror $flag" &&
2114        compile_prog "-Werror $flag" ""; then
2115       QEMU_CFLAGS="$QEMU_CFLAGS $flag"
2116       QEMU_LDFLAGS="$QEMU_LDFLAGS $flag"
2117       sp_on=1
2118       break
2119     fi
2120   done
2121   if test "$stack_protector" = yes; then
2122     if test $sp_on = 0; then
2123       error_exit "Stack protector not supported"
2124     fi
2125   fi
2126 fi
2127
2128 # Disable -Wmissing-braces on older compilers that warn even for
2129 # the "universal" C zero initializer {0}.
2130 cat > $TMPC << EOF
2131 struct {
2132   int a[2];
2133 } x = {0};
2134 EOF
2135 if compile_object "-Werror" "" ; then
2136   :
2137 else
2138   QEMU_CFLAGS="$QEMU_CFLAGS -Wno-missing-braces"
2139 fi
2140
2141 # Our module code doesn't support Windows
2142 if test "$modules" = "yes" && test "$mingw32" = "yes" ; then
2143   error_exit "Modules are not available for Windows"
2144 fi
2145
2146 # module_upgrades is only reasonable if modules are enabled
2147 if test "$modules" = "no" && test "$module_upgrades" = "yes" ; then
2148   error_exit "Can't enable module-upgrades as Modules are not enabled"
2149 fi
2150
2151 # Static linking is not possible with modules or PIE
2152 if test "$static" = "yes" ; then
2153   if test "$modules" = "yes" ; then
2154     error_exit "static and modules are mutually incompatible"
2155   fi
2156 fi
2157
2158 # Unconditional check for compiler __thread support
2159   cat > $TMPC << EOF
2160 static __thread int tls_var;
2161 int main(void) { return tls_var; }
2162 EOF
2163
2164 if ! compile_prog "-Werror" "" ; then
2165     error_exit "Your compiler does not support the __thread specifier for " \
2166         "Thread-Local Storage (TLS). Please upgrade to a version that does."
2167 fi
2168
2169 cat > $TMPC << EOF
2170
2171 #ifdef __linux__
2172 #  define THREAD __thread
2173 #else
2174 #  define THREAD
2175 #endif
2176 static THREAD int tls_var;
2177 int main(void) { return tls_var; }
2178 EOF
2179
2180 # Check we support --no-pie first; we will need this for building ROMs.
2181 if compile_prog "-Werror -fno-pie" "-no-pie"; then
2182   CFLAGS_NOPIE="-fno-pie"
2183 fi
2184
2185 if test "$static" = "yes"; then
2186   if test "$pie" != "no" && compile_prog "-Werror -fPIE -DPIE" "-static-pie"; then
2187     CONFIGURE_CFLAGS="-fPIE -DPIE $CONFIGURE_CFLAGS"
2188     QEMU_LDFLAGS="-static-pie $QEMU_LDFLAGS"
2189     pie="yes"
2190   elif test "$pie" = "yes"; then
2191     error_exit "-static-pie not available due to missing toolchain support"
2192   else
2193     QEMU_LDFLAGS="-static $QEMU_LDFLAGS"
2194     pie="no"
2195   fi
2196 elif test "$pie" = "no"; then
2197   CONFIGURE_CFLAGS="$CFLAGS_NOPIE $CONFIGURE_CFLAGS"
2198 elif compile_prog "-Werror -fPIE -DPIE" "-pie"; then
2199   CONFIGURE_CFLAGS="-fPIE -DPIE $CONFIGURE_CFLAGS"
2200   CONFIGURE_LDFLAGS="-pie $CONFIGURE_LDFLAGS"
2201   pie="yes"
2202 elif test "$pie" = "yes"; then
2203   error_exit "PIE not available due to missing toolchain support"
2204 else
2205   echo "Disabling PIE due to missing toolchain support"
2206   pie="no"
2207 fi
2208
2209 # Detect support for PT_GNU_RELRO + DT_BIND_NOW.
2210 # The combination is known as "full relro", because .got.plt is read-only too.
2211 if compile_prog "" "-Wl,-z,relro -Wl,-z,now" ; then
2212   QEMU_LDFLAGS="-Wl,-z,relro -Wl,-z,now $QEMU_LDFLAGS"
2213 fi
2214
2215 ##########################################
2216 # __sync_fetch_and_and requires at least -march=i486. Many toolchains
2217 # use i686 as default anyway, but for those that don't, an explicit
2218 # specification is necessary
2219
2220 if test "$cpu" = "i386"; then
2221   cat > $TMPC << EOF
2222 static int sfaa(int *ptr)
2223 {
2224   return __sync_fetch_and_and(ptr, 0);
2225 }
2226
2227 int main(void)
2228 {
2229   int val = 42;
2230   val = __sync_val_compare_and_swap(&val, 0, 1);
2231   sfaa(&val);
2232   return val;
2233 }
2234 EOF
2235   if ! compile_prog "" "" ; then
2236     QEMU_CFLAGS="-march=i486 $QEMU_CFLAGS"
2237   fi
2238 fi
2239
2240 #########################################
2241 # Solaris specific configure tool chain decisions
2242
2243 if test "$solaris" = "yes" ; then
2244   if has ar; then
2245     :
2246   else
2247     if test -f /usr/ccs/bin/ar ; then
2248       error_exit "No path includes ar" \
2249           "Add /usr/ccs/bin to your path and rerun configure"
2250     fi
2251     error_exit "No path includes ar"
2252   fi
2253 fi
2254
2255 if test -z "${target_list+xxx}" ; then
2256     default_targets=yes
2257     for target in $default_target_list; do
2258         target_list="$target_list $target"
2259     done
2260     target_list="${target_list# }"
2261 else
2262     default_targets=no
2263     target_list=$(echo "$target_list" | sed -e 's/,/ /g')
2264     for target in $target_list; do
2265         # Check that we recognised the target name; this allows a more
2266         # friendly error message than if we let it fall through.
2267         case " $default_target_list " in
2268             *" $target "*)
2269                 ;;
2270             *)
2271                 error_exit "Unknown target name '$target'"
2272                 ;;
2273         esac
2274     done
2275 fi
2276
2277 for target in $target_list; do
2278     # if a deprecated target is enabled we note it here
2279     if echo "$deprecated_targets_list" | grep -q "$target"; then
2280         add_to deprecated_features $target
2281     fi
2282 done
2283
2284 # see if system emulation was really requested
2285 case " $target_list " in
2286   *"-softmmu "*) softmmu=yes
2287   ;;
2288   *) softmmu=no
2289   ;;
2290 esac
2291
2292 feature_not_found() {
2293   feature=$1
2294   remedy=$2
2295
2296   error_exit "User requested feature $feature" \
2297       "configure was not able to find it." \
2298       "$remedy"
2299 }
2300
2301 # ---
2302 # big/little endian test
2303 cat > $TMPC << EOF
2304 short big_endian[] = { 0x4269, 0x4765, 0x4e64, 0x4961, 0x4e00, 0, };
2305 short little_endian[] = { 0x694c, 0x7454, 0x654c, 0x6e45, 0x6944, 0x6e41, 0, };
2306 extern int foo(short *, short *);
2307 int main(int argc, char *argv[]) {
2308     return foo(big_endian, little_endian);
2309 }
2310 EOF
2311
2312 if compile_object ; then
2313     if strings -a $TMPO | grep -q BiGeNdIaN ; then
2314         bigendian="yes"
2315     elif strings -a $TMPO | grep -q LiTtLeEnDiAn ; then
2316         bigendian="no"
2317     else
2318         echo big/little test failed
2319     fi
2320 else
2321     echo big/little test failed
2322 fi
2323
2324 ##########################################
2325 # system tools
2326 if test -z "$want_tools"; then
2327     if test "$softmmu" = "no"; then
2328         want_tools=no
2329     else
2330         want_tools=yes
2331     fi
2332 fi
2333
2334 ##########################################
2335 # cocoa implies not SDL or GTK
2336 # (the cocoa UI code currently assumes it is always the active UI
2337 # and doesn't interact well with other UI frontend code)
2338 if test "$cocoa" = "enabled"; then
2339     if test "$sdl" = "enabled"; then
2340         error_exit "Cocoa and SDL UIs cannot both be enabled at once"
2341     fi
2342     if test "$gtk" = "yes"; then
2343         error_exit "Cocoa and GTK UIs cannot both be enabled at once"
2344     fi
2345     gtk=no
2346     sdl=disabled
2347 fi
2348
2349 # Some versions of Mac OS X incorrectly define SIZE_MAX
2350 cat > $TMPC << EOF
2351 #include <stdint.h>
2352 #include <stdio.h>
2353 int main(int argc, char *argv[]) {
2354     return printf("%zu", SIZE_MAX);
2355 }
2356 EOF
2357 have_broken_size_max=no
2358 if ! compile_object -Werror ; then
2359     have_broken_size_max=yes
2360 fi
2361
2362 ##########################################
2363 # L2TPV3 probe
2364
2365 cat > $TMPC <<EOF
2366 #include <sys/socket.h>
2367 #include <linux/ip.h>
2368 int main(void) { return sizeof(struct mmsghdr); }
2369 EOF
2370 if compile_prog "" "" ; then
2371   l2tpv3=yes
2372 else
2373   l2tpv3=no
2374 fi
2375
2376 cat > $TMPC <<EOF
2377 #include <sys/mman.h>
2378 int main(int argc, char *argv[]) {
2379     return mlockall(MCL_FUTURE);
2380 }
2381 EOF
2382 if compile_prog "" "" ; then
2383   have_mlockall=yes
2384 else
2385   have_mlockall=no
2386 fi
2387
2388 #########################################
2389 # vhost interdependencies and host support
2390
2391 # vhost backends
2392 if test "$vhost_user" = "yes" && test "$linux" != "yes"; then
2393   error_exit "vhost-user is only available on Linux"
2394 fi
2395 test "$vhost_vdpa" = "" && vhost_vdpa=$linux
2396 if test "$vhost_vdpa" = "yes" && test "$linux" != "yes"; then
2397   error_exit "vhost-vdpa is only available on Linux"
2398 fi
2399 test "$vhost_kernel" = "" && vhost_kernel=$linux
2400 if test "$vhost_kernel" = "yes" && test "$linux" != "yes"; then
2401   error_exit "vhost-kernel is only available on Linux"
2402 fi
2403
2404 # vhost-kernel devices
2405 test "$vhost_scsi" = "" && vhost_scsi=$vhost_kernel
2406 if test "$vhost_scsi" = "yes" && test "$vhost_kernel" != "yes"; then
2407   error_exit "--enable-vhost-scsi requires --enable-vhost-kernel"
2408 fi
2409 test "$vhost_vsock" = "" && vhost_vsock=$vhost_kernel
2410 if test "$vhost_vsock" = "yes" && test "$vhost_kernel" != "yes"; then
2411   error_exit "--enable-vhost-vsock requires --enable-vhost-kernel"
2412 fi
2413
2414 # vhost-user backends
2415 test "$vhost_net_user" = "" && vhost_net_user=$vhost_user
2416 if test "$vhost_net_user" = "yes" && test "$vhost_user" = "no"; then
2417   error_exit "--enable-vhost-net-user requires --enable-vhost-user"
2418 fi
2419 test "$vhost_crypto" = "" && vhost_crypto=$vhost_user
2420 if test "$vhost_crypto" = "yes" && test "$vhost_user" = "no"; then
2421   error_exit "--enable-vhost-crypto requires --enable-vhost-user"
2422 fi
2423 test "$vhost_user_fs" = "" && vhost_user_fs=$vhost_user
2424 if test "$vhost_user_fs" = "yes" && test "$vhost_user" = "no"; then
2425   error_exit "--enable-vhost-user-fs requires --enable-vhost-user"
2426 fi
2427 #vhost-vdpa backends
2428 test "$vhost_net_vdpa" = "" && vhost_net_vdpa=$vhost_vdpa
2429 if test "$vhost_net_vdpa" = "yes" && test "$vhost_vdpa" = "no"; then
2430   error_exit "--enable-vhost-net-vdpa requires --enable-vhost-vdpa"
2431 fi
2432
2433 # OR the vhost-kernel, vhost-vdpa and vhost-user values for simplicity
2434 if test "$vhost_net" = ""; then
2435   test "$vhost_net_user" = "yes" && vhost_net=yes
2436   test "$vhost_net_vdpa" = "yes" && vhost_net=yes
2437   test "$vhost_kernel" = "yes" && vhost_net=yes
2438 fi
2439
2440 ##########################################
2441 # pkg-config probe
2442
2443 if ! has "$pkg_config_exe"; then
2444   error_exit "pkg-config binary '$pkg_config_exe' not found"
2445 fi
2446
2447 ##########################################
2448 # NPTL probe
2449
2450 if test "$linux_user" = "yes"; then
2451   cat > $TMPC <<EOF
2452 #include <sched.h>
2453 #include <linux/futex.h>
2454 int main(void) {
2455 #if !defined(CLONE_SETTLS) || !defined(FUTEX_WAIT)
2456 #error bork
2457 #endif
2458   return 0;
2459 }
2460 EOF
2461   if ! compile_object ; then
2462     feature_not_found "nptl" "Install glibc and linux kernel headers."
2463   fi
2464 fi
2465
2466 ##########################################
2467 # lzo check
2468
2469 if test "$lzo" != "no" ; then
2470     cat > $TMPC << EOF
2471 #include <lzo/lzo1x.h>
2472 int main(void) { lzo_version(); return 0; }
2473 EOF
2474     if compile_prog "" "-llzo2" ; then
2475         lzo_libs="-llzo2"
2476         lzo="yes"
2477     else
2478         if test "$lzo" = "yes"; then
2479             feature_not_found "liblzo2" "Install liblzo2 devel"
2480         fi
2481         lzo="no"
2482     fi
2483 fi
2484
2485 ##########################################
2486 # snappy check
2487
2488 if test "$snappy" != "no" ; then
2489     cat > $TMPC << EOF
2490 #include <snappy-c.h>
2491 int main(void) { snappy_max_compressed_length(4096); return 0; }
2492 EOF
2493     if compile_prog "" "-lsnappy" ; then
2494         snappy_libs='-lsnappy'
2495         snappy="yes"
2496     else
2497         if test "$snappy" = "yes"; then
2498             feature_not_found "libsnappy" "Install libsnappy devel"
2499         fi
2500         snappy="no"
2501     fi
2502 fi
2503
2504 ##########################################
2505 # bzip2 check
2506
2507 if test "$bzip2" != "no" ; then
2508     cat > $TMPC << EOF
2509 #include <bzlib.h>
2510 int main(void) { BZ2_bzlibVersion(); return 0; }
2511 EOF
2512     if compile_prog "" "-lbz2" ; then
2513         bzip2="yes"
2514     else
2515         if test "$bzip2" = "yes"; then
2516             feature_not_found "libbzip2" "Install libbzip2 devel"
2517         fi
2518         bzip2="no"
2519     fi
2520 fi
2521
2522 ##########################################
2523 # lzfse check
2524
2525 if test "$lzfse" != "no" ; then
2526     cat > $TMPC << EOF
2527 #include <lzfse.h>
2528 int main(void) { lzfse_decode_scratch_size(); return 0; }
2529 EOF
2530     if compile_prog "" "-llzfse" ; then
2531         lzfse="yes"
2532     else
2533         if test "$lzfse" = "yes"; then
2534             feature_not_found "lzfse" "Install lzfse devel"
2535         fi
2536         lzfse="no"
2537     fi
2538 fi
2539
2540 ##########################################
2541 # zstd check
2542
2543 if test "$zstd" != "no" ; then
2544     libzstd_minver="1.4.0"
2545     if $pkg_config --atleast-version=$libzstd_minver libzstd ; then
2546         zstd_cflags="$($pkg_config --cflags libzstd)"
2547         zstd_libs="$($pkg_config --libs libzstd)"
2548         zstd="yes"
2549     else
2550         if test "$zstd" = "yes" ; then
2551             feature_not_found "libzstd" "Install libzstd devel"
2552         fi
2553         zstd="no"
2554     fi
2555 fi
2556
2557 ##########################################
2558 # libseccomp check
2559
2560 if test "$seccomp" != "no" ; then
2561     libseccomp_minver="2.3.0"
2562     if $pkg_config --atleast-version=$libseccomp_minver libseccomp ; then
2563         seccomp_cflags="$($pkg_config --cflags libseccomp)"
2564         seccomp_libs="$($pkg_config --libs libseccomp)"
2565         seccomp="yes"
2566     else
2567         if test "$seccomp" = "yes" ; then
2568             feature_not_found "libseccomp" \
2569                  "Install libseccomp devel >= $libseccomp_minver"
2570         fi
2571         seccomp="no"
2572     fi
2573 fi
2574
2575 ##########################################
2576 # xen probe
2577
2578 if test "$xen" != "disabled" ; then
2579   # Check whether Xen library path is specified via --extra-ldflags to avoid
2580   # overriding this setting with pkg-config output. If not, try pkg-config
2581   # to obtain all needed flags.
2582
2583   if ! echo $EXTRA_LDFLAGS | grep tools/libxc > /dev/null && \
2584      $pkg_config --exists xencontrol ; then
2585     xen_ctrl_version="$(printf '%d%02d%02d' \
2586       $($pkg_config --modversion xencontrol | sed 's/\./ /g') )"
2587     xen=enabled
2588     xen_pc="xencontrol xenstore xenforeignmemory xengnttab"
2589     xen_pc="$xen_pc xenevtchn xendevicemodel"
2590     if $pkg_config --exists xentoolcore; then
2591       xen_pc="$xen_pc xentoolcore"
2592     fi
2593     xen_cflags="$($pkg_config --cflags $xen_pc)"
2594     xen_libs="$($pkg_config --libs $xen_pc)"
2595   else
2596
2597     xen_libs="-lxenstore -lxenctrl"
2598     xen_stable_libs="-lxenforeignmemory -lxengnttab -lxenevtchn"
2599
2600     # First we test whether Xen headers and libraries are available.
2601     # If no, we are done and there is no Xen support.
2602     # If yes, more tests are run to detect the Xen version.
2603
2604     # Xen (any)
2605     cat > $TMPC <<EOF
2606 #include <xenctrl.h>
2607 int main(void) {
2608   return 0;
2609 }
2610 EOF
2611     if ! compile_prog "" "$xen_libs" ; then
2612       # Xen not found
2613       if test "$xen" = "enabled" ; then
2614         feature_not_found "xen" "Install xen devel"
2615       fi
2616       xen=disabled
2617
2618     # Xen unstable
2619     elif
2620         cat > $TMPC <<EOF &&
2621 #undef XC_WANT_COMPAT_DEVICEMODEL_API
2622 #define __XEN_TOOLS__
2623 #include <xendevicemodel.h>
2624 #include <xenforeignmemory.h>
2625 int main(void) {
2626   xendevicemodel_handle *xd;
2627   xenforeignmemory_handle *xfmem;
2628
2629   xd = xendevicemodel_open(0, 0);
2630   xendevicemodel_pin_memory_cacheattr(xd, 0, 0, 0, 0);
2631
2632   xfmem = xenforeignmemory_open(0, 0);
2633   xenforeignmemory_map_resource(xfmem, 0, 0, 0, 0, 0, NULL, 0, 0);
2634
2635   return 0;
2636 }
2637 EOF
2638         compile_prog "" "$xen_libs -lxendevicemodel $xen_stable_libs -lxentoolcore"
2639       then
2640       xen_stable_libs="-lxendevicemodel $xen_stable_libs -lxentoolcore"
2641       xen_ctrl_version=41100
2642       xen=enabled
2643     elif
2644         cat > $TMPC <<EOF &&
2645 #undef XC_WANT_COMPAT_MAP_FOREIGN_API
2646 #include <xenforeignmemory.h>
2647 #include <xentoolcore.h>
2648 int main(void) {
2649   xenforeignmemory_handle *xfmem;
2650
2651   xfmem = xenforeignmemory_open(0, 0);
2652   xenforeignmemory_map2(xfmem, 0, 0, 0, 0, 0, 0, 0);
2653   xentoolcore_restrict_all(0);
2654
2655   return 0;
2656 }
2657 EOF
2658         compile_prog "" "$xen_libs -lxendevicemodel $xen_stable_libs -lxentoolcore"
2659       then
2660       xen_stable_libs="-lxendevicemodel $xen_stable_libs -lxentoolcore"
2661       xen_ctrl_version=41000
2662       xen=enabled
2663     elif
2664         cat > $TMPC <<EOF &&
2665 #undef XC_WANT_COMPAT_DEVICEMODEL_API
2666 #define __XEN_TOOLS__
2667 #include <xendevicemodel.h>
2668 int main(void) {
2669   xendevicemodel_handle *xd;
2670
2671   xd = xendevicemodel_open(0, 0);
2672   xendevicemodel_close(xd);
2673
2674   return 0;
2675 }
2676 EOF
2677         compile_prog "" "$xen_libs -lxendevicemodel $xen_stable_libs"
2678       then
2679       xen_stable_libs="-lxendevicemodel $xen_stable_libs"
2680       xen_ctrl_version=40900
2681       xen=enabled
2682     elif
2683         cat > $TMPC <<EOF &&
2684 /*
2685  * If we have stable libs the we don't want the libxc compat
2686  * layers, regardless of what CFLAGS we may have been given.
2687  *
2688  * Also, check if xengnttab_grant_copy_segment_t is defined and
2689  * grant copy operation is implemented.
2690  */
2691 #undef XC_WANT_COMPAT_EVTCHN_API
2692 #undef XC_WANT_COMPAT_GNTTAB_API
2693 #undef XC_WANT_COMPAT_MAP_FOREIGN_API
2694 #include <xenctrl.h>
2695 #include <xenstore.h>
2696 #include <xenevtchn.h>
2697 #include <xengnttab.h>
2698 #include <xenforeignmemory.h>
2699 #include <stdint.h>
2700 #include <xen/hvm/hvm_info_table.h>
2701 #if !defined(HVM_MAX_VCPUS)
2702 # error HVM_MAX_VCPUS not defined
2703 #endif
2704 int main(void) {
2705   xc_interface *xc = NULL;
2706   xenforeignmemory_handle *xfmem;
2707   xenevtchn_handle *xe;
2708   xengnttab_handle *xg;
2709   xengnttab_grant_copy_segment_t* seg = NULL;
2710
2711   xs_daemon_open();
2712
2713   xc = xc_interface_open(0, 0, 0);
2714   xc_hvm_set_mem_type(0, 0, HVMMEM_ram_ro, 0, 0);
2715   xc_domain_add_to_physmap(0, 0, XENMAPSPACE_gmfn, 0, 0);
2716   xc_hvm_inject_msi(xc, 0, 0xf0000000, 0x00000000);
2717   xc_hvm_create_ioreq_server(xc, 0, HVM_IOREQSRV_BUFIOREQ_ATOMIC, NULL);
2718
2719   xfmem = xenforeignmemory_open(0, 0);
2720   xenforeignmemory_map(xfmem, 0, 0, 0, 0, 0);
2721
2722   xe = xenevtchn_open(0, 0);
2723   xenevtchn_fd(xe);
2724
2725   xg = xengnttab_open(0, 0);
2726   xengnttab_grant_copy(xg, 0, seg);
2727
2728   return 0;
2729 }
2730 EOF
2731         compile_prog "" "$xen_libs $xen_stable_libs"
2732       then
2733       xen_ctrl_version=40800
2734       xen=enabled
2735     elif
2736         cat > $TMPC <<EOF &&
2737 /*
2738  * If we have stable libs the we don't want the libxc compat
2739  * layers, regardless of what CFLAGS we may have been given.
2740  */
2741 #undef XC_WANT_COMPAT_EVTCHN_API
2742 #undef XC_WANT_COMPAT_GNTTAB_API
2743 #undef XC_WANT_COMPAT_MAP_FOREIGN_API
2744 #include <xenctrl.h>
2745 #include <xenstore.h>
2746 #include <xenevtchn.h>
2747 #include <xengnttab.h>
2748 #include <xenforeignmemory.h>
2749 #include <stdint.h>
2750 #include <xen/hvm/hvm_info_table.h>
2751 #if !defined(HVM_MAX_VCPUS)
2752 # error HVM_MAX_VCPUS not defined
2753 #endif
2754 int main(void) {
2755   xc_interface *xc = NULL;
2756   xenforeignmemory_handle *xfmem;
2757   xenevtchn_handle *xe;
2758   xengnttab_handle *xg;
2759
2760   xs_daemon_open();
2761
2762   xc = xc_interface_open(0, 0, 0);
2763   xc_hvm_set_mem_type(0, 0, HVMMEM_ram_ro, 0, 0);
2764   xc_domain_add_to_physmap(0, 0, XENMAPSPACE_gmfn, 0, 0);
2765   xc_hvm_inject_msi(xc, 0, 0xf0000000, 0x00000000);
2766   xc_hvm_create_ioreq_server(xc, 0, HVM_IOREQSRV_BUFIOREQ_ATOMIC, NULL);
2767
2768   xfmem = xenforeignmemory_open(0, 0);
2769   xenforeignmemory_map(xfmem, 0, 0, 0, 0, 0);
2770
2771   xe = xenevtchn_open(0, 0);
2772   xenevtchn_fd(xe);
2773
2774   xg = xengnttab_open(0, 0);
2775   xengnttab_map_grant_ref(xg, 0, 0, 0);
2776
2777   return 0;
2778 }
2779 EOF
2780         compile_prog "" "$xen_libs $xen_stable_libs"
2781       then
2782       xen_ctrl_version=40701
2783       xen=enabled
2784
2785     # Xen 4.6
2786     elif
2787         cat > $TMPC <<EOF &&
2788 #include <xenctrl.h>
2789 #include <xenstore.h>
2790 #include <stdint.h>
2791 #include <xen/hvm/hvm_info_table.h>
2792 #if !defined(HVM_MAX_VCPUS)
2793 # error HVM_MAX_VCPUS not defined
2794 #endif
2795 int main(void) {
2796   xc_interface *xc;
2797   xs_daemon_open();
2798   xc = xc_interface_open(0, 0, 0);
2799   xc_hvm_set_mem_type(0, 0, HVMMEM_ram_ro, 0, 0);
2800   xc_gnttab_open(NULL, 0);
2801   xc_domain_add_to_physmap(0, 0, XENMAPSPACE_gmfn, 0, 0);
2802   xc_hvm_inject_msi(xc, 0, 0xf0000000, 0x00000000);
2803   xc_hvm_create_ioreq_server(xc, 0, HVM_IOREQSRV_BUFIOREQ_ATOMIC, NULL);
2804   xc_reserved_device_memory_map(xc, 0, 0, 0, 0, NULL, 0);
2805   return 0;
2806 }
2807 EOF
2808         compile_prog "" "$xen_libs"
2809       then
2810       xen_ctrl_version=40600
2811       xen=enabled
2812
2813     # Xen 4.5
2814     elif
2815         cat > $TMPC <<EOF &&
2816 #include <xenctrl.h>
2817 #include <xenstore.h>
2818 #include <stdint.h>
2819 #include <xen/hvm/hvm_info_table.h>
2820 #if !defined(HVM_MAX_VCPUS)
2821 # error HVM_MAX_VCPUS not defined
2822 #endif
2823 int main(void) {
2824   xc_interface *xc;
2825   xs_daemon_open();
2826   xc = xc_interface_open(0, 0, 0);
2827   xc_hvm_set_mem_type(0, 0, HVMMEM_ram_ro, 0, 0);
2828   xc_gnttab_open(NULL, 0);
2829   xc_domain_add_to_physmap(0, 0, XENMAPSPACE_gmfn, 0, 0);
2830   xc_hvm_inject_msi(xc, 0, 0xf0000000, 0x00000000);
2831   xc_hvm_create_ioreq_server(xc, 0, 0, NULL);
2832   return 0;
2833 }
2834 EOF
2835         compile_prog "" "$xen_libs"
2836       then
2837       xen_ctrl_version=40500
2838       xen=enabled
2839
2840     elif
2841         cat > $TMPC <<EOF &&
2842 #include <xenctrl.h>
2843 #include <xenstore.h>
2844 #include <stdint.h>
2845 #include <xen/hvm/hvm_info_table.h>
2846 #if !defined(HVM_MAX_VCPUS)
2847 # error HVM_MAX_VCPUS not defined
2848 #endif
2849 int main(void) {
2850   xc_interface *xc;
2851   xs_daemon_open();
2852   xc = xc_interface_open(0, 0, 0);
2853   xc_hvm_set_mem_type(0, 0, HVMMEM_ram_ro, 0, 0);
2854   xc_gnttab_open(NULL, 0);
2855   xc_domain_add_to_physmap(0, 0, XENMAPSPACE_gmfn, 0, 0);
2856   xc_hvm_inject_msi(xc, 0, 0xf0000000, 0x00000000);
2857   return 0;
2858 }
2859 EOF
2860         compile_prog "" "$xen_libs"
2861       then
2862       xen_ctrl_version=40200
2863       xen=enabled
2864
2865     else
2866       if test "$xen" = "enabled" ; then
2867         feature_not_found "xen (unsupported version)" \
2868                           "Install a supported xen (xen 4.2 or newer)"
2869       fi
2870       xen=disabled
2871     fi
2872
2873     if test "$xen" = enabled; then
2874       if test $xen_ctrl_version -ge 40701  ; then
2875         xen_libs="$xen_libs $xen_stable_libs "
2876       fi
2877     fi
2878   fi
2879 fi
2880
2881 ##########################################
2882 # X11 probe
2883 if $pkg_config --exists "x11"; then
2884     have_x11=yes
2885     x11_cflags=$($pkg_config --cflags x11)
2886     x11_libs=$($pkg_config --libs x11)
2887 fi
2888
2889 ##########################################
2890 # GTK probe
2891
2892 if test "$gtk" != "no"; then
2893     gtkpackage="gtk+-3.0"
2894     gtkx11package="gtk+-x11-3.0"
2895     gtkversion="3.22.0"
2896     if $pkg_config --exists "$gtkpackage >= $gtkversion"; then
2897         gtk_cflags=$($pkg_config --cflags $gtkpackage)
2898         gtk_libs=$($pkg_config --libs $gtkpackage)
2899         gtk_version=$($pkg_config --modversion $gtkpackage)
2900         if $pkg_config --exists "$gtkx11package >= $gtkversion"; then
2901             need_x11=yes
2902             gtk_cflags="$gtk_cflags $x11_cflags"
2903             gtk_libs="$gtk_libs $x11_libs"
2904         fi
2905         gtk="yes"
2906     elif test "$gtk" = "yes"; then
2907         feature_not_found "gtk" "Install gtk3-devel"
2908     else
2909         gtk="no"
2910     fi
2911 fi
2912
2913
2914 ##########################################
2915 # GNUTLS probe
2916
2917 if test "$gnutls" != "no"; then
2918     pass="no"
2919     if $pkg_config --exists "gnutls >= 3.1.18"; then
2920         gnutls_cflags=$($pkg_config --cflags gnutls)
2921         gnutls_libs=$($pkg_config --libs gnutls)
2922         # Packaging for the static libraries is not always correct.
2923         # At least ubuntu 18.04 ships only shared libraries.
2924         write_c_skeleton
2925         if compile_prog "" "$gnutls_libs" ; then
2926             pass="yes"
2927         fi
2928     fi
2929     if test "$pass" = "no" && test "$gnutls" = "yes"; then
2930         feature_not_found "gnutls" "Install gnutls devel >= 3.1.18"
2931     else
2932         gnutls="$pass"
2933     fi
2934 fi
2935
2936
2937 # If user didn't give a --disable/enable-gcrypt flag,
2938 # then mark as disabled if user requested nettle
2939 # explicitly
2940 if test -z "$gcrypt"
2941 then
2942     if test "$nettle" = "yes"
2943     then
2944         gcrypt="no"
2945     fi
2946 fi
2947
2948 # If user didn't give a --disable/enable-nettle flag,
2949 # then mark as disabled if user requested gcrypt
2950 # explicitly
2951 if test -z "$nettle"
2952 then
2953     if test "$gcrypt" = "yes"
2954     then
2955         nettle="no"
2956     fi
2957 fi
2958
2959 has_libgcrypt() {
2960     if ! has "libgcrypt-config"
2961     then
2962         return 1
2963     fi
2964
2965     if test -n "$cross_prefix"
2966     then
2967         host=$(libgcrypt-config --host)
2968         if test "$host-" != $cross_prefix
2969         then
2970             return 1
2971         fi
2972     fi
2973
2974     maj=`libgcrypt-config --version | awk -F . '{print $1}'`
2975     min=`libgcrypt-config --version | awk -F . '{print $2}'`
2976
2977     if test $maj != 1 || test $min -lt 5
2978     then
2979        return 1
2980     fi
2981
2982     return 0
2983 }
2984
2985
2986 if test "$nettle" != "no"; then
2987     pass="no"
2988     if $pkg_config --exists "nettle >= 2.7.1"; then
2989         nettle_cflags=$($pkg_config --cflags nettle)
2990         nettle_libs=$($pkg_config --libs nettle)
2991         nettle_version=$($pkg_config --modversion nettle)
2992         # Link test to make sure the given libraries work (e.g for static).
2993         write_c_skeleton
2994         if compile_prog "" "$nettle_libs" ; then
2995             if test -z "$gcrypt"; then
2996                gcrypt="no"
2997             fi
2998             pass="yes"
2999         fi
3000     fi
3001     if test "$pass" = "yes"
3002     then
3003         cat > $TMPC << EOF
3004 #include <nettle/xts.h>
3005 int main(void) {
3006   return 0;
3007 }
3008 EOF
3009         if compile_prog "$nettle_cflags" "$nettle_libs" ; then
3010             nettle_xts=yes
3011             qemu_private_xts=no
3012         fi
3013     fi
3014     if test "$pass" = "no" && test "$nettle" = "yes"; then
3015         feature_not_found "nettle" "Install nettle devel >= 2.7.1"
3016     else
3017         nettle="$pass"
3018     fi
3019 fi
3020
3021 if test "$gcrypt" != "no"; then
3022     pass="no"
3023     if has_libgcrypt; then
3024         gcrypt_cflags=$(libgcrypt-config --cflags)
3025         gcrypt_libs=$(libgcrypt-config --libs)
3026         # Debian has removed -lgpg-error from libgcrypt-config
3027         # as it "spreads unnecessary dependencies" which in
3028         # turn breaks static builds...
3029         if test "$static" = "yes"
3030         then
3031             gcrypt_libs="$gcrypt_libs -lgpg-error"
3032         fi
3033
3034         # Link test to make sure the given libraries work (e.g for static).
3035         write_c_skeleton
3036         if compile_prog "" "$gcrypt_libs" ; then
3037             pass="yes"
3038         fi
3039     fi
3040     if test "$pass" = "yes"; then
3041         gcrypt="yes"
3042         cat > $TMPC << EOF
3043 #include <gcrypt.h>
3044 int main(void) {
3045   gcry_mac_hd_t handle;
3046   gcry_mac_open(&handle, GCRY_MAC_HMAC_MD5,
3047                 GCRY_MAC_FLAG_SECURE, NULL);
3048   return 0;
3049 }
3050 EOF
3051         if compile_prog "$gcrypt_cflags" "$gcrypt_libs" ; then
3052             gcrypt_hmac=yes
3053         fi
3054         cat > $TMPC << EOF
3055 #include <gcrypt.h>
3056 int main(void) {
3057   gcry_cipher_hd_t handle;
3058   gcry_cipher_open(&handle, GCRY_CIPHER_AES, GCRY_CIPHER_MODE_XTS, 0);
3059   return 0;
3060 }
3061 EOF
3062         if compile_prog "$gcrypt_cflags" "$gcrypt_libs" ; then
3063             gcrypt_xts=yes
3064             qemu_private_xts=no
3065         fi
3066     elif test "$gcrypt" = "yes"; then
3067         feature_not_found "gcrypt" "Install gcrypt devel >= 1.5.0"
3068     else
3069         gcrypt="no"
3070     fi
3071 fi
3072
3073
3074 if test "$gcrypt" = "yes" && test "$nettle" = "yes"
3075 then
3076     error_exit "Only one of gcrypt & nettle can be enabled"
3077 fi
3078
3079 ##########################################
3080 # libtasn1 - only for the TLS creds/session test suite
3081
3082 tasn1=yes
3083 tasn1_cflags=""
3084 tasn1_libs=""
3085 if $pkg_config --exists "libtasn1"; then
3086     tasn1_cflags=$($pkg_config --cflags libtasn1)
3087     tasn1_libs=$($pkg_config --libs libtasn1)
3088 else
3089     tasn1=no
3090 fi
3091
3092
3093 ##########################################
3094 # PAM probe
3095
3096 if test "$auth_pam" != "no"; then
3097     cat > $TMPC <<EOF
3098 #include <security/pam_appl.h>
3099 #include <stdio.h>
3100 int main(void) {
3101    const char *service_name = "qemu";
3102    const char *user = "frank";
3103    const struct pam_conv pam_conv = { 0 };
3104    pam_handle_t *pamh = NULL;
3105    pam_start(service_name, user, &pam_conv, &pamh);
3106    return 0;
3107 }
3108 EOF
3109     if compile_prog "" "-lpam" ; then
3110         auth_pam=yes
3111     else
3112         if test "$auth_pam" = "yes"; then
3113             feature_not_found "PAM" "Install PAM development package"
3114         else
3115             auth_pam=no
3116         fi
3117     fi
3118 fi
3119
3120 ##########################################
3121 # VTE probe
3122
3123 if test "$vte" != "no"; then
3124     vteminversion="0.32.0"
3125     if $pkg_config --exists "vte-2.91"; then
3126       vtepackage="vte-2.91"
3127     else
3128       vtepackage="vte-2.90"
3129     fi
3130     if $pkg_config --exists "$vtepackage >= $vteminversion"; then
3131         vte_cflags=$($pkg_config --cflags $vtepackage)
3132         vte_libs=$($pkg_config --libs $vtepackage)
3133         vteversion=$($pkg_config --modversion $vtepackage)
3134         vte="yes"
3135     elif test "$vte" = "yes"; then
3136         feature_not_found "vte" "Install libvte-2.90/2.91 devel"
3137     else
3138         vte="no"
3139     fi
3140 fi
3141
3142 ##########################################
3143 # RDMA needs OpenFabrics libraries
3144 if test "$rdma" != "no" ; then
3145   cat > $TMPC <<EOF
3146 #include <rdma/rdma_cma.h>
3147 int main(void) { return 0; }
3148 EOF
3149   rdma_libs="-lrdmacm -libverbs -libumad"
3150   if compile_prog "" "$rdma_libs" ; then
3151     rdma="yes"
3152   else
3153     if test "$rdma" = "yes" ; then
3154         error_exit \
3155             " OpenFabrics librdmacm/libibverbs/libibumad not present." \
3156             " Your options:" \
3157             "  (1) Fast: Install infiniband packages (devel) from your distro." \
3158             "  (2) Cleanest: Install libraries from www.openfabrics.org" \
3159             "  (3) Also: Install softiwarp if you don't have RDMA hardware"
3160     fi
3161     rdma="no"
3162   fi
3163 fi
3164
3165 ##########################################
3166 # PVRDMA detection
3167
3168 cat > $TMPC <<EOF &&
3169 #include <sys/mman.h>
3170
3171 int
3172 main(void)
3173 {
3174     char buf = 0;
3175     void *addr = &buf;
3176     addr = mremap(addr, 0, 1, MREMAP_MAYMOVE | MREMAP_FIXED);
3177
3178     return 0;
3179 }
3180 EOF
3181
3182 if test "$rdma" = "yes" ; then
3183     case "$pvrdma" in
3184     "")
3185         if compile_prog "" ""; then
3186             pvrdma="yes"
3187         else
3188             pvrdma="no"
3189         fi
3190         ;;
3191     "yes")
3192         if ! compile_prog "" ""; then
3193             error_exit "PVRDMA is not supported since mremap is not implemented"
3194         fi
3195         pvrdma="yes"
3196         ;;
3197     "no")
3198         pvrdma="no"
3199         ;;
3200     esac
3201 else
3202     if test "$pvrdma" = "yes" ; then
3203         error_exit "PVRDMA requires rdma suppport"
3204     fi
3205     pvrdma="no"
3206 fi
3207
3208 # Let's see if enhanced reg_mr is supported
3209 if test "$pvrdma" = "yes" ; then
3210
3211 cat > $TMPC <<EOF &&
3212 #include <infiniband/verbs.h>
3213
3214 int
3215 main(void)
3216 {
3217     struct ibv_mr *mr;
3218     struct ibv_pd *pd = NULL;
3219     size_t length = 10;
3220     uint64_t iova = 0;
3221     int access = 0;
3222     void *addr = NULL;
3223
3224     mr = ibv_reg_mr_iova(pd, addr, length, iova, access);
3225
3226     ibv_dereg_mr(mr);
3227
3228     return 0;
3229 }
3230 EOF
3231     if ! compile_prog "" "-libverbs"; then
3232         QEMU_CFLAGS="$QEMU_CFLAGS -DLEGACY_RDMA_REG_MR"
3233     fi
3234 fi
3235
3236 ##########################################
3237 # xfsctl() probe, used for file-posix.c
3238 if test "$xfs" != "no" ; then
3239   cat > $TMPC << EOF
3240 #include <stddef.h>  /* NULL */
3241 #include <xfs/xfs.h>
3242 int main(void)
3243 {
3244     xfsctl(NULL, 0, 0, NULL);
3245     return 0;
3246 }
3247 EOF
3248   if compile_prog "" "" ; then
3249     xfs="yes"
3250   else
3251     if test "$xfs" = "yes" ; then
3252       feature_not_found "xfs" "Install xfsprogs/xfslibs devel"
3253     fi
3254     xfs=no
3255   fi
3256 fi
3257
3258 ##########################################
3259 # vde libraries probe
3260 if test "$vde" != "no" ; then
3261   vde_libs="-lvdeplug"
3262   cat > $TMPC << EOF
3263 #include <libvdeplug.h>
3264 int main(void)
3265 {
3266     struct vde_open_args a = {0, 0, 0};
3267     char s[] = "";
3268     vde_open(s, s, &a);
3269     return 0;
3270 }
3271 EOF
3272   if compile_prog "" "$vde_libs" ; then
3273     vde=yes
3274   else
3275     if test "$vde" = "yes" ; then
3276       feature_not_found "vde" "Install vde (Virtual Distributed Ethernet) devel"
3277     fi
3278     vde=no
3279   fi
3280 fi
3281
3282 ##########################################
3283 # netmap support probe
3284 # Apart from looking for netmap headers, we make sure that the host API version
3285 # supports the netmap backend (>=11). The upper bound (15) is meant to simulate
3286 # a minor/major version number. Minor new features will be marked with values up
3287 # to 15, and if something happens that requires a change to the backend we will
3288 # move above 15, submit the backend fixes and modify this two bounds.
3289 if test "$netmap" != "no" ; then
3290   cat > $TMPC << EOF
3291 #include <inttypes.h>
3292 #include <net/if.h>
3293 #include <net/netmap.h>
3294 #include <net/netmap_user.h>
3295 #if (NETMAP_API < 11) || (NETMAP_API > 15)
3296 #error
3297 #endif
3298 int main(void) { return 0; }
3299 EOF
3300   if compile_prog "" "" ; then
3301     netmap=yes
3302   else
3303     if test "$netmap" = "yes" ; then
3304       feature_not_found "netmap"
3305     fi
3306     netmap=no
3307   fi
3308 fi
3309
3310 ##########################################
3311 # libcap-ng library probe
3312 if test "$cap_ng" != "no" ; then
3313   cap_libs="-lcap-ng"
3314   cat > $TMPC << EOF
3315 #include <cap-ng.h>
3316 int main(void)
3317 {
3318     capng_capability_to_name(CAPNG_EFFECTIVE);
3319     return 0;
3320 }
3321 EOF
3322   if compile_prog "" "$cap_libs" ; then
3323     cap_ng=yes
3324   else
3325     if test "$cap_ng" = "yes" ; then
3326       feature_not_found "cap_ng" "Install libcap-ng devel"
3327     fi
3328     cap_ng=no
3329   fi
3330 fi
3331
3332 ##########################################
3333 # Sound support libraries probe
3334
3335 audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/,/ /g')
3336 for drv in $audio_drv_list; do
3337     case $drv in
3338     alsa | try-alsa)
3339     if $pkg_config alsa --exists; then
3340         alsa_libs=$($pkg_config alsa --libs)
3341         alsa_cflags=$($pkg_config alsa --cflags)
3342         alsa=yes
3343         if test "$drv" = "try-alsa"; then
3344             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-alsa/alsa/')
3345         fi
3346     else
3347         if test "$drv" = "try-alsa"; then
3348             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-alsa//')
3349         else
3350             error_exit "$drv check failed" \
3351                 "Make sure to have the $drv libs and headers installed."
3352         fi
3353     fi
3354     ;;
3355
3356     pa | try-pa)
3357     if $pkg_config libpulse --exists; then
3358         libpulse=yes
3359         pulse_libs=$($pkg_config libpulse --libs)
3360         pulse_cflags=$($pkg_config libpulse --cflags)
3361         if test "$drv" = "try-pa"; then
3362             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-pa/pa/')
3363         fi
3364     else
3365         if test "$drv" = "try-pa"; then
3366             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-pa//')
3367         else
3368             error_exit "$drv check failed" \
3369                 "Make sure to have the $drv libs and headers installed."
3370         fi
3371     fi
3372     ;;
3373
3374     sdl)
3375     if test "$sdl" = "no"; then
3376         error_exit "sdl not found or disabled, can not use sdl audio driver"
3377     fi
3378     ;;
3379
3380     try-sdl)
3381     if test "$sdl" = "no"; then
3382         audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-sdl//')
3383     else
3384         audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-sdl/sdl/')
3385     fi
3386     ;;
3387
3388     coreaudio)
3389       coreaudio_libs="-framework CoreAudio"
3390     ;;
3391
3392     dsound)
3393       dsound_libs="-lole32 -ldxguid"
3394       audio_win_int="yes"
3395     ;;
3396
3397     oss)
3398       oss_libs="$oss_lib"
3399     ;;
3400
3401     jack | try-jack)
3402     if $pkg_config jack --exists; then
3403         libjack=yes
3404         jack_libs=$($pkg_config jack --libs)
3405         if test "$drv" = "try-jack"; then
3406             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-jack/jack/')
3407         fi
3408     else
3409         if test "$drv" = "try-jack"; then
3410             audio_drv_list=$(echo "$audio_drv_list" | sed -e 's/try-jack//')
3411         else
3412             error_exit "$drv check failed" \
3413                 "Make sure to have the $drv libs and headers installed."
3414         fi
3415     fi
3416     ;;
3417
3418     *)
3419     echo "$audio_possible_drivers" | grep -q "\<$drv\>" || {
3420         error_exit "Unknown driver '$drv' selected" \
3421             "Possible drivers are: $audio_possible_drivers"
3422     }
3423     ;;
3424     esac
3425 done
3426
3427 ##########################################
3428 # BrlAPI probe
3429
3430 if test "$brlapi" != "no" ; then
3431   brlapi_libs="-lbrlapi"
3432   cat > $TMPC << EOF
3433 #include <brlapi.h>
3434 #include <stddef.h>
3435 int main( void ) { return brlapi__openConnection (NULL, NULL, NULL); }
3436 EOF
3437   if compile_prog "" "$brlapi_libs" ; then
3438     brlapi=yes
3439   else
3440     if test "$brlapi" = "yes" ; then
3441       feature_not_found "brlapi" "Install brlapi devel"
3442     fi
3443     brlapi=no
3444   fi
3445 fi
3446
3447 ##########################################
3448 # curl probe
3449 if test "$curl" != "no" ; then
3450   if $pkg_config libcurl --exists; then
3451     curlconfig="$pkg_config libcurl"
3452   else
3453     curlconfig=curl-config
3454   fi
3455   cat > $TMPC << EOF
3456 #include <curl/curl.h>
3457 int main(void) { curl_easy_init(); curl_multi_setopt(0, 0, 0); return 0; }
3458 EOF
3459   curl_cflags=$($curlconfig --cflags 2>/dev/null)
3460   curl_libs=$($curlconfig --libs 2>/dev/null)
3461   if compile_prog "$curl_cflags" "$curl_libs" ; then
3462     curl=yes
3463   else
3464     if test "$curl" = "yes" ; then
3465       feature_not_found "curl" "Install libcurl devel"
3466     fi
3467     curl=no
3468   fi
3469 fi # test "$curl"
3470
3471 ##########################################
3472 # glib support probe
3473
3474 glib_req_ver=2.48
3475 glib_modules=gthread-2.0
3476 if test "$modules" = yes; then
3477     glib_modules="$glib_modules gmodule-export-2.0"
3478 fi
3479 if test "$plugins" = yes; then
3480     glib_modules="$glib_modules gmodule-2.0"
3481 fi
3482
3483 for i in $glib_modules; do
3484     if $pkg_config --atleast-version=$glib_req_ver $i; then
3485         glib_cflags=$($pkg_config --cflags $i)
3486         glib_libs=$($pkg_config --libs $i)
3487     else
3488         error_exit "glib-$glib_req_ver $i is required to compile QEMU"
3489     fi
3490 done
3491
3492 # This workaround is required due to a bug in pkg-config file for glib as it
3493 # doesn't define GLIB_STATIC_COMPILATION for pkg-config --static
3494
3495 if test "$static" = yes && test "$mingw32" = yes; then
3496     glib_cflags="-DGLIB_STATIC_COMPILATION $glib_cflags"
3497 fi
3498
3499 if $pkg_config --atleast-version=$glib_req_ver gio-2.0; then
3500     gio_cflags=$($pkg_config --cflags gio-2.0)
3501     gio_libs=$($pkg_config --libs gio-2.0)
3502     gdbus_codegen=$($pkg_config --variable=gdbus_codegen gio-2.0)
3503     if [ ! -x "$gdbus_codegen" ]; then
3504         gdbus_codegen=
3505     fi
3506     # Check that the libraries actually work -- Ubuntu 18.04 ships
3507     # with pkg-config --static --libs data for gio-2.0 that is missing
3508     # -lblkid and will give a link error.
3509     cat > $TMPC <<EOF
3510 #include <gio/gio.h>
3511 int main(void)
3512 {
3513     g_dbus_proxy_new_sync(0, 0, 0, 0, 0, 0, 0, 0);
3514     return 0;
3515 }
3516 EOF
3517     if compile_prog "$gio_cflags" "$gio_libs" ; then
3518         gio=yes
3519     else
3520         gio=no
3521     fi
3522 else
3523     gio=no
3524 fi
3525
3526 if $pkg_config --atleast-version=$glib_req_ver gio-unix-2.0; then
3527     gio_cflags="$gio_cflags $($pkg_config --cflags gio-unix-2.0)"
3528     gio_libs="$gio_libs $($pkg_config --libs gio-unix-2.0)"
3529 fi
3530
3531 # Sanity check that the current size_t matches the
3532 # size that glib thinks it should be. This catches
3533 # problems on multi-arch where people try to build
3534 # 32-bit QEMU while pointing at 64-bit glib headers
3535 cat > $TMPC <<EOF
3536 #include <glib.h>
3537 #include <unistd.h>
3538
3539 #define QEMU_BUILD_BUG_ON(x) \
3540   typedef char qemu_build_bug_on[(x)?-1:1] __attribute__((unused));
3541
3542 int main(void) {
3543    QEMU_BUILD_BUG_ON(sizeof(size_t) != GLIB_SIZEOF_SIZE_T);
3544    return 0;
3545 }
3546 EOF
3547
3548 if ! compile_prog "$glib_cflags" "$glib_libs" ; then
3549     error_exit "sizeof(size_t) doesn't match GLIB_SIZEOF_SIZE_T."\
3550                "You probably need to set PKG_CONFIG_LIBDIR"\
3551                "to point to the right pkg-config files for your"\
3552                "build target"
3553 fi
3554
3555 # Silence clang 3.5.0 warnings about glib attribute __alloc_size__ usage
3556 cat > $TMPC << EOF
3557 #include <glib.h>
3558 int main(void) { return 0; }
3559 EOF
3560 if ! compile_prog "$glib_cflags -Werror" "$glib_libs" ; then
3561     if cc_has_warning_flag "-Wno-unknown-attributes"; then
3562         glib_cflags="-Wno-unknown-attributes $glib_cflags"
3563         CONFIGURE_CFLAGS="-Wno-unknown-attributes $CONFIGURE_CFLAGS"
3564     fi
3565 fi
3566
3567 # Silence clang warnings triggered by glib < 2.57.2
3568 cat > $TMPC << EOF
3569 #include <glib.h>
3570 typedef struct Foo {
3571     int i;
3572 } Foo;
3573 static void foo_free(Foo *f)
3574 {
3575     g_free(f);
3576 }
3577 G_DEFINE_AUTOPTR_CLEANUP_FUNC(Foo, foo_free);
3578 int main(void) { return 0; }
3579 EOF
3580 if ! compile_prog "$glib_cflags -Werror" "$glib_libs" ; then
3581     if cc_has_warning_flag "-Wno-unused-function"; then
3582         glib_cflags="$glib_cflags -Wno-unused-function"
3583         CONFIGURE_CFLAGS="$CONFIGURE_CFLAGS -Wno-unused-function"
3584     fi
3585 fi
3586
3587 ##########################################
3588 # SHA command probe for modules
3589 if test "$modules" = yes; then
3590     shacmd_probe="sha1sum sha1 shasum"
3591     for c in $shacmd_probe; do
3592         if has $c; then
3593             shacmd="$c"
3594             break
3595         fi
3596     done
3597     if test "$shacmd" = ""; then
3598         error_exit "one of the checksum commands is required to enable modules: $shacmd_probe"
3599     fi
3600 fi
3601
3602 ##########################################
3603 # pthread probe
3604 PTHREADLIBS_LIST="-pthread -lpthread -lpthreadGC2"
3605
3606 pthread=no
3607 cat > $TMPC << EOF
3608 #include <pthread.h>
3609 static void *f(void *p) { return NULL; }
3610 int main(void) {
3611   pthread_t thread;
3612   pthread_create(&thread, 0, f, 0);
3613   return 0;
3614 }
3615 EOF
3616 if compile_prog "" "" ; then
3617   pthread=yes
3618 else
3619   for pthread_lib in $PTHREADLIBS_LIST; do
3620     if compile_prog "" "$pthread_lib" ; then
3621       pthread=yes
3622       found=no
3623       for lib_entry in $LIBS; do
3624         if test "$lib_entry" = "$pthread_lib"; then
3625           found=yes
3626           break
3627         fi
3628       done
3629       if test "$found" = "no"; then
3630         LIBS="$pthread_lib $LIBS"
3631       fi
3632       break
3633     fi
3634   done
3635 fi
3636
3637 if test "$mingw32" != yes && test "$pthread" = no; then
3638   error_exit "pthread check failed" \
3639       "Make sure to have the pthread libs and headers installed."
3640 fi
3641
3642 # check for pthread_setname_np with thread id
3643 pthread_setname_np_w_tid=no
3644 cat > $TMPC << EOF
3645 #include <pthread.h>
3646
3647 static void *f(void *p) { return NULL; }
3648 int main(void)
3649 {
3650     pthread_t thread;
3651     pthread_create(&thread, 0, f, 0);
3652     pthread_setname_np(thread, "QEMU");
3653     return 0;
3654 }
3655 EOF
3656 if compile_prog "" "$pthread_lib" ; then
3657   pthread_setname_np_w_tid=yes
3658 fi
3659
3660 # check for pthread_setname_np without thread id
3661 pthread_setname_np_wo_tid=no
3662 cat > $TMPC << EOF
3663 #include <pthread.h>
3664
3665 static void *f(void *p) { pthread_setname_np("QEMU"); return NULL; }
3666 int main(void)
3667 {
3668     pthread_t thread;
3669     pthread_create(&thread, 0, f, 0);
3670     return 0;
3671 }
3672 EOF
3673 if compile_prog "" "$pthread_lib" ; then
3674   pthread_setname_np_wo_tid=yes
3675 fi
3676
3677 ##########################################
3678 # rbd probe
3679 if test "$rbd" != "no" ; then
3680   cat > $TMPC <<EOF
3681 #include <stdio.h>
3682 #include <rbd/librbd.h>
3683 int main(void) {
3684     rados_t cluster;
3685     rados_create(&cluster, NULL);
3686     return 0;
3687 }
3688 EOF
3689   rbd_libs="-lrbd -lrados"
3690   if compile_prog "" "$rbd_libs" ; then
3691     rbd=yes
3692   else
3693     if test "$rbd" = "yes" ; then
3694       feature_not_found "rados block device" "Install librbd/ceph devel"
3695     fi
3696     rbd=no
3697   fi
3698 fi
3699
3700 ##########################################
3701 # libssh probe
3702 if test "$libssh" != "no" ; then
3703   if $pkg_config --exists libssh; then
3704     libssh_cflags=$($pkg_config libssh --cflags)
3705     libssh_libs=$($pkg_config libssh --libs)
3706     libssh=yes
3707   else
3708     if test "$libssh" = "yes" ; then
3709       error_exit "libssh required for --enable-libssh"
3710     fi
3711     libssh=no
3712   fi
3713 fi
3714
3715 ##########################################
3716 # Check for libssh 0.8
3717 # This is done like this instead of using the LIBSSH_VERSION_* and
3718 # SSH_VERSION_* macros because some distributions in the past shipped
3719 # snapshots of the future 0.8 from Git, and those snapshots did not
3720 # have updated version numbers (still referring to 0.7.0).
3721
3722 if test "$libssh" = "yes"; then
3723   cat > $TMPC <<EOF
3724 #include <libssh/libssh.h>
3725 int main(void) { return ssh_get_server_publickey(NULL, NULL); }
3726 EOF
3727   if compile_prog "$libssh_cflags" "$libssh_libs"; then
3728     libssh_cflags="-DHAVE_LIBSSH_0_8 $libssh_cflags"
3729   fi
3730 fi
3731
3732 ##########################################
3733 # linux-aio probe
3734
3735 if test "$linux_aio" != "no" ; then
3736   cat > $TMPC <<EOF
3737 #include <libaio.h>
3738 #include <sys/eventfd.h>
3739 #include <stddef.h>
3740 int main(void) { io_setup(0, NULL); io_set_eventfd(NULL, 0); eventfd(0, 0); return 0; }
3741 EOF
3742   if compile_prog "" "-laio" ; then
3743     linux_aio=yes
3744   else
3745     if test "$linux_aio" = "yes" ; then
3746       feature_not_found "linux AIO" "Install libaio devel"
3747     fi
3748     linux_aio=no
3749   fi
3750 fi
3751 ##########################################
3752 # linux-io-uring probe
3753
3754 if test "$linux_io_uring" != "no" ; then
3755   if $pkg_config liburing; then
3756     linux_io_uring_cflags=$($pkg_config --cflags liburing)
3757     linux_io_uring_libs=$($pkg_config --libs liburing)
3758     linux_io_uring=yes
3759   else
3760     if test "$linux_io_uring" = "yes" ; then
3761       feature_not_found "linux io_uring" "Install liburing devel"
3762     fi
3763     linux_io_uring=no
3764   fi
3765 fi
3766
3767 ##########################################
3768 # TPM emulation is only on POSIX
3769
3770 if test "$tpm" = ""; then
3771   if test "$mingw32" = "yes"; then
3772     tpm=no
3773   else
3774     tpm=yes
3775   fi
3776 elif test "$tpm" = "yes"; then
3777   if test "$mingw32" = "yes" ; then
3778     error_exit "TPM emulation only available on POSIX systems"
3779   fi
3780 fi
3781
3782 ##########################################
3783 # attr probe
3784
3785 libattr_libs=
3786 if test "$attr" != "no" ; then
3787   cat > $TMPC <<EOF
3788 #include <stdio.h>
3789 #include <sys/types.h>
3790 #ifdef CONFIG_LIBATTR
3791 #include <attr/xattr.h>
3792 #else
3793 #include <sys/xattr.h>
3794 #endif
3795 int main(void) { getxattr(NULL, NULL, NULL, 0); setxattr(NULL, NULL, NULL, 0, 0); return 0; }
3796 EOF
3797   if compile_prog "" "" ; then
3798     attr=yes
3799   # Older distros have <attr/xattr.h>, and need -lattr:
3800   elif compile_prog "-DCONFIG_LIBATTR" "-lattr" ; then
3801     attr=yes
3802     libattr_libs="-lattr"
3803     libattr=yes
3804   else
3805     if test "$attr" = "yes" ; then
3806       feature_not_found "ATTR" "Install libc6 or libattr devel"
3807     fi
3808     attr=no
3809   fi
3810 fi
3811
3812 ##########################################
3813 # iovec probe
3814 cat > $TMPC <<EOF
3815 #include <sys/types.h>
3816 #include <sys/uio.h>
3817 #include <unistd.h>
3818 int main(void) { return sizeof(struct iovec); }
3819 EOF
3820 iovec=no
3821 if compile_prog "" "" ; then
3822   iovec=yes
3823 fi
3824
3825 ##########################################
3826 # preadv probe
3827 cat > $TMPC <<EOF
3828 #include <sys/types.h>
3829 #include <sys/uio.h>
3830 #include <unistd.h>
3831 int main(void) { return preadv(0, 0, 0, 0); }
3832 EOF
3833 preadv=no
3834 if compile_prog "" "" ; then
3835   preadv=yes
3836 fi
3837
3838 ##########################################
3839 # fdt probe
3840
3841 case "$fdt" in
3842   auto | enabled | internal)
3843     # Simpler to always update submodule, even if not needed.
3844     if test -e "${source_path}/.git" && test $git_update = 'yes' ; then
3845       git_submodules="${git_submodules} dtc"
3846     fi
3847     ;;
3848 esac
3849
3850 ##########################################
3851 # opengl probe (for sdl2, gtk, milkymist-tmu2)
3852
3853 gbm="no"
3854 if $pkg_config gbm; then
3855     gbm_cflags="$($pkg_config --cflags gbm)"
3856     gbm_libs="$($pkg_config --libs gbm)"
3857     gbm="yes"
3858 fi
3859
3860 if test "$opengl" != "no" ; then
3861   opengl_pkgs="epoxy gbm"
3862   if $pkg_config $opengl_pkgs; then
3863     opengl_cflags="$($pkg_config --cflags $opengl_pkgs)"
3864     opengl_libs="$($pkg_config --libs $opengl_pkgs)"
3865     opengl=yes
3866     if test "$gtk" = "yes" && $pkg_config --exists "$gtkpackage >= 3.16"; then
3867         gtk_gl="yes"
3868     fi
3869   else
3870     if test "$opengl" = "yes" ; then
3871       feature_not_found "opengl" "Please install opengl (mesa) devel pkgs: $opengl_pkgs"
3872     fi
3873     opengl_cflags=""
3874     opengl_libs=""
3875     opengl=no
3876   fi
3877 fi
3878
3879 if test "$opengl" = "yes"; then
3880   cat > $TMPC << EOF
3881 #include <epoxy/egl.h>
3882 #ifndef EGL_MESA_image_dma_buf_export
3883 # error mesa/epoxy lacks support for dmabufs (mesa 10.6+)
3884 #endif
3885 int main(void) { return 0; }
3886 EOF
3887   if compile_prog "" "" ; then
3888     opengl_dmabuf=yes
3889   fi
3890 fi
3891
3892 if test "$opengl" = "yes" && test "$have_x11" = "yes"; then
3893   for target in $target_list; do
3894     case $target in
3895       lm32-softmmu) # milkymist-tmu2 requires X11 and OpenGL
3896         need_x11=yes
3897       ;;
3898     esac
3899   done
3900 fi
3901
3902 ##########################################
3903 # libxml2 probe
3904 if test "$libxml2" != "no" ; then
3905     if $pkg_config --exists libxml-2.0; then
3906         libxml2="yes"
3907         libxml2_cflags=$($pkg_config --cflags libxml-2.0)
3908         libxml2_libs=$($pkg_config --libs libxml-2.0)
3909     else
3910         if test "$libxml2" = "yes"; then
3911             feature_not_found "libxml2" "Install libxml2 devel"
3912         fi
3913         libxml2="no"
3914     fi
3915 fi
3916
3917 ##########################################
3918 # glusterfs probe
3919 if test "$glusterfs" != "no" ; then
3920   if $pkg_config --atleast-version=3 glusterfs-api; then
3921     glusterfs="yes"
3922     glusterfs_cflags=$($pkg_config --cflags glusterfs-api)
3923     glusterfs_libs=$($pkg_config --libs glusterfs-api)
3924     if $pkg_config --atleast-version=4 glusterfs-api; then
3925       glusterfs_xlator_opt="yes"
3926     fi
3927     if $pkg_config --atleast-version=5 glusterfs-api; then
3928       glusterfs_discard="yes"
3929     fi
3930     if $pkg_config --atleast-version=6 glusterfs-api; then
3931       glusterfs_fallocate="yes"
3932       glusterfs_zerofill="yes"
3933     fi
3934     cat > $TMPC << EOF
3935 #include <glusterfs/api/glfs.h>
3936
3937 int
3938 main(void)
3939 {
3940         /* new glfs_ftruncate() passes two additional args */
3941         return glfs_ftruncate(NULL, 0, NULL, NULL);
3942 }
3943 EOF
3944     if compile_prog "$glusterfs_cflags" "$glusterfs_libs" ; then
3945       glusterfs_ftruncate_has_stat="yes"
3946     fi
3947     cat > $TMPC << EOF
3948 #include <glusterfs/api/glfs.h>
3949
3950 /* new glfs_io_cbk() passes two additional glfs_stat structs */
3951 static void
3952 glusterfs_iocb(glfs_fd_t *fd, ssize_t ret, struct glfs_stat *prestat, struct glfs_stat *poststat, void *data)
3953 {}
3954
3955 int
3956 main(void)
3957 {
3958         glfs_io_cbk iocb = &glusterfs_iocb;
3959         iocb(NULL, 0 , NULL, NULL, NULL);
3960         return 0;
3961 }
3962 EOF
3963     if compile_prog "$glusterfs_cflags" "$glusterfs_libs" ; then
3964       glusterfs_iocb_has_stat="yes"
3965     fi
3966   else
3967     if test "$glusterfs" = "yes" ; then
3968       feature_not_found "GlusterFS backend support" \
3969           "Install glusterfs-api devel >= 3"
3970     fi
3971     glusterfs="no"
3972   fi
3973 fi
3974
3975 # Check for inotify functions when we are building linux-user
3976 # emulator.  This is done because older glibc versions don't
3977 # have syscall stubs for these implemented.  In that case we
3978 # don't provide them even if kernel supports them.
3979 #
3980 inotify=no
3981 cat > $TMPC << EOF
3982 #include <sys/inotify.h>
3983
3984 int
3985 main(void)
3986 {
3987         /* try to start inotify */
3988         return inotify_init();
3989 }
3990 EOF
3991 if compile_prog "" "" ; then
3992   inotify=yes
3993 fi
3994
3995 inotify1=no
3996 cat > $TMPC << EOF
3997 #include <sys/inotify.h>
3998
3999 int
4000 main(void)
4001 {
4002     /* try to start inotify */
4003     return inotify_init1(0);
4004 }
4005 EOF
4006 if compile_prog "" "" ; then
4007   inotify1=yes
4008 fi
4009
4010 # check if pipe2 is there
4011 pipe2=no
4012 cat > $TMPC << EOF
4013 #include <unistd.h>
4014 #include <fcntl.h>
4015
4016 int main(void)
4017 {
4018     int pipefd[2];
4019     return pipe2(pipefd, O_CLOEXEC);
4020 }
4021 EOF
4022 if compile_prog "" "" ; then
4023   pipe2=yes
4024 fi
4025
4026 # check if accept4 is there
4027 accept4=no
4028 cat > $TMPC << EOF
4029 #include <sys/socket.h>
4030 #include <stddef.h>
4031
4032 int main(void)
4033 {
4034     accept4(0, NULL, NULL, SOCK_CLOEXEC);
4035     return 0;
4036 }
4037 EOF
4038 if compile_prog "" "" ; then
4039   accept4=yes
4040 fi
4041
4042 # check if tee/splice is there. vmsplice was added same time.
4043 splice=no
4044 cat > $TMPC << EOF
4045 #include <unistd.h>
4046 #include <fcntl.h>
4047 #include <limits.h>
4048
4049 int main(void)
4050 {
4051     int len, fd = 0;
4052     len = tee(STDIN_FILENO, STDOUT_FILENO, INT_MAX, SPLICE_F_NONBLOCK);
4053     splice(STDIN_FILENO, NULL, fd, NULL, len, SPLICE_F_MOVE);
4054     return 0;
4055 }
4056 EOF
4057 if compile_prog "" "" ; then
4058   splice=yes
4059 fi
4060
4061 ##########################################
4062 # libnuma probe
4063
4064 if test "$numa" != "no" ; then
4065   cat > $TMPC << EOF
4066 #include <numa.h>
4067 int main(void) { return numa_available(); }
4068 EOF
4069
4070   if compile_prog "" "-lnuma" ; then
4071     numa=yes
4072     numa_libs="-lnuma"
4073   else
4074     if test "$numa" = "yes" ; then
4075       feature_not_found "numa" "install numactl devel"
4076     fi
4077     numa=no
4078   fi
4079 fi
4080
4081 malloc=system
4082 if test "$tcmalloc" = "yes" && test "$jemalloc" = "yes" ; then
4083     echo "ERROR: tcmalloc && jemalloc can't be used at the same time"
4084     exit 1
4085 elif test "$tcmalloc" = "yes" ; then
4086     malloc=tcmalloc
4087 elif test "$jemalloc" = "yes" ; then
4088     malloc=jemalloc
4089 fi
4090
4091 ##########################################
4092 # signalfd probe
4093 signalfd="no"
4094 cat > $TMPC << EOF
4095 #include <unistd.h>
4096 #include <sys/syscall.h>
4097 #include <signal.h>
4098 int main(void) { return syscall(SYS_signalfd, -1, NULL, _NSIG / 8); }
4099 EOF
4100
4101 if compile_prog "" "" ; then
4102   signalfd=yes
4103 fi
4104
4105 # check if optreset global is declared by <getopt.h>
4106 optreset="no"
4107 cat > $TMPC << EOF
4108 #include <getopt.h>
4109 int main(void) { return optreset; }
4110 EOF
4111
4112 if compile_prog "" "" ; then
4113   optreset=yes
4114 fi
4115
4116 # check if eventfd is supported
4117 eventfd=no
4118 cat > $TMPC << EOF
4119 #include <sys/eventfd.h>
4120
4121 int main(void)
4122 {
4123     return eventfd(0, EFD_NONBLOCK | EFD_CLOEXEC);
4124 }
4125 EOF
4126 if compile_prog "" "" ; then
4127   eventfd=yes
4128 fi
4129
4130 # check if memfd is supported
4131 memfd=no
4132 cat > $TMPC << EOF
4133 #include <sys/mman.h>
4134
4135 int main(void)
4136 {
4137     return memfd_create("foo", MFD_ALLOW_SEALING);
4138 }
4139 EOF
4140 if compile_prog "" "" ; then
4141   memfd=yes
4142 fi
4143
4144 # check for usbfs
4145 have_usbfs=no
4146 if test "$linux_user" = "yes"; then
4147   cat > $TMPC << EOF
4148 #include <linux/usbdevice_fs.h>
4149
4150 #ifndef USBDEVFS_GET_CAPABILITIES
4151 #error "USBDEVFS_GET_CAPABILITIES undefined"
4152 #endif
4153
4154 #ifndef USBDEVFS_DISCONNECT_CLAIM
4155 #error "USBDEVFS_DISCONNECT_CLAIM undefined"
4156 #endif
4157
4158 int main(void)
4159 {
4160     return 0;
4161 }
4162 EOF
4163   if compile_prog "" ""; then
4164     have_usbfs=yes
4165   fi
4166 fi
4167
4168 # check for fallocate
4169 fallocate=no
4170 cat > $TMPC << EOF
4171 #include <fcntl.h>
4172
4173 int main(void)
4174 {
4175     fallocate(0, 0, 0, 0);
4176     return 0;
4177 }
4178 EOF
4179 if compile_prog "" "" ; then
4180   fallocate=yes
4181 fi
4182
4183 # check for fallocate hole punching
4184 fallocate_punch_hole=no
4185 cat > $TMPC << EOF
4186 #include <fcntl.h>
4187 #include <linux/falloc.h>
4188
4189 int main(void)
4190 {
4191     fallocate(0, FALLOC_FL_PUNCH_HOLE | FALLOC_FL_KEEP_SIZE, 0, 0);
4192     return 0;
4193 }
4194 EOF
4195 if compile_prog "" "" ; then
4196   fallocate_punch_hole=yes
4197 fi
4198
4199 # check that fallocate supports range zeroing inside the file
4200 fallocate_zero_range=no
4201 cat > $TMPC << EOF
4202 #include <fcntl.h>
4203 #include <linux/falloc.h>
4204
4205 int main(void)
4206 {
4207     fallocate(0, FALLOC_FL_ZERO_RANGE, 0, 0);
4208     return 0;
4209 }
4210 EOF
4211 if compile_prog "" "" ; then
4212   fallocate_zero_range=yes
4213 fi
4214
4215 # check for posix_fallocate
4216 posix_fallocate=no
4217 cat > $TMPC << EOF
4218 #include <fcntl.h>
4219
4220 int main(void)
4221 {
4222     posix_fallocate(0, 0, 0);
4223     return 0;
4224 }
4225 EOF
4226 if compile_prog "" "" ; then
4227     posix_fallocate=yes
4228 fi
4229
4230 # check for sync_file_range
4231 sync_file_range=no
4232 cat > $TMPC << EOF
4233 #include <fcntl.h>
4234
4235 int main(void)
4236 {
4237     sync_file_range(0, 0, 0, 0);
4238     return 0;
4239 }
4240 EOF
4241 if compile_prog "" "" ; then
4242   sync_file_range=yes
4243 fi
4244
4245 # check for linux/fiemap.h and FS_IOC_FIEMAP
4246 fiemap=no
4247 cat > $TMPC << EOF
4248 #include <sys/ioctl.h>
4249 #include <linux/fs.h>
4250 #include <linux/fiemap.h>
4251
4252 int main(void)
4253 {
4254     ioctl(0, FS_IOC_FIEMAP, 0);
4255     return 0;
4256 }
4257 EOF
4258 if compile_prog "" "" ; then
4259   fiemap=yes
4260 fi
4261
4262 # check for dup3
4263 dup3=no
4264 cat > $TMPC << EOF
4265 #include <unistd.h>
4266
4267 int main(void)
4268 {
4269     dup3(0, 0, 0);
4270     return 0;
4271 }
4272 EOF
4273 if compile_prog "" "" ; then
4274   dup3=yes
4275 fi
4276
4277 # check for ppoll support
4278 ppoll=no
4279 cat > $TMPC << EOF
4280 #include <poll.h>
4281
4282 int main(void)
4283 {
4284     struct pollfd pfd = { .fd = 0, .events = 0, .revents = 0 };
4285     ppoll(&pfd, 1, 0, 0);
4286     return 0;
4287 }
4288 EOF
4289 if compile_prog "" "" ; then
4290   ppoll=yes
4291 fi
4292
4293 # check for prctl(PR_SET_TIMERSLACK , ... ) support
4294 prctl_pr_set_timerslack=no
4295 cat > $TMPC << EOF
4296 #include <sys/prctl.h>
4297
4298 int main(void)
4299 {
4300     prctl(PR_SET_TIMERSLACK, 1, 0, 0, 0);
4301     return 0;
4302 }
4303 EOF
4304 if compile_prog "" "" ; then
4305   prctl_pr_set_timerslack=yes
4306 fi
4307
4308 # check for epoll support
4309 epoll=no
4310 cat > $TMPC << EOF
4311 #include <sys/epoll.h>
4312
4313 int main(void)
4314 {
4315     epoll_create(0);
4316     return 0;
4317 }
4318 EOF
4319 if compile_prog "" "" ; then
4320   epoll=yes
4321 fi
4322
4323 # epoll_create1 is a later addition
4324 # so we must check separately for its presence
4325 epoll_create1=no
4326 cat > $TMPC << EOF
4327 #include <sys/epoll.h>
4328
4329 int main(void)
4330 {
4331     /* Note that we use epoll_create1 as a value, not as
4332      * a function being called. This is necessary so that on
4333      * old SPARC glibc versions where the function was present in
4334      * the library but not declared in the header file we will
4335      * fail the configure check. (Otherwise we will get a compiler
4336      * warning but not an error, and will proceed to fail the
4337      * qemu compile where we compile with -Werror.)
4338      */
4339     return (int)(uintptr_t)&epoll_create1;
4340 }
4341 EOF
4342 if compile_prog "" "" ; then
4343   epoll_create1=yes
4344 fi
4345
4346 # check for sendfile support
4347 sendfile=no
4348 cat > $TMPC << EOF
4349 #include <sys/sendfile.h>
4350
4351 int main(void)
4352 {
4353     return sendfile(0, 0, 0, 0);
4354 }
4355 EOF
4356 if compile_prog "" "" ; then
4357   sendfile=yes
4358 fi
4359
4360 # check for timerfd support (glibc 2.8 and newer)
4361 timerfd=no
4362 cat > $TMPC << EOF
4363 #include <sys/timerfd.h>
4364
4365 int main(void)
4366 {
4367     return(timerfd_create(CLOCK_REALTIME, 0));
4368 }
4369 EOF
4370 if compile_prog "" "" ; then
4371   timerfd=yes
4372 fi
4373
4374 # check for setns and unshare support
4375 setns=no
4376 cat > $TMPC << EOF
4377 #include <sched.h>
4378
4379 int main(void)
4380 {
4381     int ret;
4382     ret = setns(0, 0);
4383     ret = unshare(0);
4384     return ret;
4385 }
4386 EOF
4387 if compile_prog "" "" ; then
4388   setns=yes
4389 fi
4390
4391 # clock_adjtime probe
4392 clock_adjtime=no
4393 cat > $TMPC <<EOF
4394 #include <time.h>
4395
4396 int main(void)
4397 {
4398     return clock_adjtime(0, 0);
4399 }
4400 EOF
4401 clock_adjtime=no
4402 if compile_prog "" "" ; then
4403   clock_adjtime=yes
4404 fi
4405
4406 # syncfs probe
4407 syncfs=no
4408 cat > $TMPC <<EOF
4409 #include <unistd.h>
4410
4411 int main(void)
4412 {
4413     return syncfs(0);
4414 }
4415 EOF
4416 syncfs=no
4417 if compile_prog "" "" ; then
4418   syncfs=yes
4419 fi
4420
4421 # Search for bswap_32 function
4422 byteswap_h=no
4423 cat > $TMPC << EOF
4424 #include <byteswap.h>
4425 int main(void) { return bswap_32(0); }
4426 EOF
4427 if compile_prog "" "" ; then
4428   byteswap_h=yes
4429 fi
4430
4431 # Search for bswap32 function
4432 bswap_h=no
4433 cat > $TMPC << EOF
4434 #include <sys/endian.h>
4435 #include <sys/types.h>
4436 #include <machine/bswap.h>
4437 int main(void) { return bswap32(0); }
4438 EOF
4439 if compile_prog "" "" ; then
4440   bswap_h=yes
4441 fi
4442
4443 ##########################################
4444 # Do we have libiscsi >= 1.9.0
4445 if test "$libiscsi" != "no" ; then
4446   if $pkg_config --atleast-version=1.9.0 libiscsi; then
4447     libiscsi="yes"
4448     libiscsi_cflags=$($pkg_config --cflags libiscsi)
4449     libiscsi_libs=$($pkg_config --libs libiscsi)
4450   else
4451     if test "$libiscsi" = "yes" ; then
4452       feature_not_found "libiscsi" "Install libiscsi >= 1.9.0"
4453     fi
4454     libiscsi="no"
4455   fi
4456 fi
4457
4458 ##########################################
4459 # Do we need librt
4460 # uClibc provides 2 versions of clock_gettime(), one with realtime
4461 # support and one without. This means that the clock_gettime() don't
4462 # need -lrt. We still need it for timer_create() so we check for this
4463 # function in addition.
4464 cat > $TMPC <<EOF
4465 #include <signal.h>
4466 #include <time.h>
4467 int main(void) {
4468   timer_create(CLOCK_REALTIME, NULL, NULL);
4469   return clock_gettime(CLOCK_REALTIME, NULL);
4470 }
4471 EOF
4472
4473 if compile_prog "" "" ; then
4474   :
4475 # we need pthread for static linking. use previous pthread test result
4476 elif compile_prog "" "$pthread_lib -lrt" ; then
4477   LIBS="$LIBS -lrt"
4478 fi
4479
4480 # Check whether we have openpty() in either libc or libutil
4481 cat > $TMPC << EOF
4482 extern int openpty(int *am, int *as, char *name, void *termp, void *winp);
4483 int main(void) { return openpty(0, 0, 0, 0, 0); }
4484 EOF
4485
4486 have_openpty="no"
4487 if compile_prog "" "" ; then
4488   have_openpty="yes"
4489 else
4490   if compile_prog "" "-lutil" ; then
4491     have_openpty="yes"
4492   fi
4493 fi
4494
4495 ##########################################
4496 # spice probe
4497 if test "$spice" != "no" ; then
4498   cat > $TMPC << EOF
4499 #include <spice.h>
4500 int main(void) { spice_server_new(); return 0; }
4501 EOF
4502   spice_cflags=$($pkg_config --cflags spice-protocol spice-server 2>/dev/null)
4503   spice_libs=$($pkg_config --libs spice-protocol spice-server 2>/dev/null)
4504   if $pkg_config --atleast-version=0.12.5 spice-server && \
4505      $pkg_config --atleast-version=0.12.3 spice-protocol && \
4506      compile_prog "$spice_cflags" "$spice_libs" ; then
4507     spice="yes"
4508   else
4509     if test "$spice" = "yes" ; then
4510       feature_not_found "spice" \
4511           "Install spice-server(>=0.12.5) and spice-protocol(>=0.12.3) devel"
4512     fi
4513     spice="no"
4514   fi
4515 fi
4516
4517 # check for smartcard support
4518 if test "$smartcard" != "no"; then
4519     if $pkg_config --atleast-version=2.5.1 libcacard; then
4520         libcacard_cflags=$($pkg_config --cflags libcacard)
4521         libcacard_libs=$($pkg_config --libs libcacard)
4522         smartcard="yes"
4523     else
4524         if test "$smartcard" = "yes"; then
4525             feature_not_found "smartcard" "Install libcacard devel"
4526         fi
4527         smartcard="no"
4528     fi
4529 fi
4530
4531 # check for libusb
4532 if test "$libusb" != "no" ; then
4533     if $pkg_config --atleast-version=1.0.13 libusb-1.0; then
4534         libusb="yes"
4535         libusb_cflags=$($pkg_config --cflags libusb-1.0)
4536         libusb_libs=$($pkg_config --libs libusb-1.0)
4537     else
4538         if test "$libusb" = "yes"; then
4539             feature_not_found "libusb" "Install libusb devel >= 1.0.13"
4540         fi
4541         libusb="no"
4542     fi
4543 fi
4544
4545 # check for usbredirparser for usb network redirection support
4546 if test "$usb_redir" != "no" ; then
4547     if $pkg_config --atleast-version=0.6 libusbredirparser-0.5; then
4548         usb_redir="yes"
4549         usb_redir_cflags=$($pkg_config --cflags libusbredirparser-0.5)
4550         usb_redir_libs=$($pkg_config --libs libusbredirparser-0.5)
4551     else
4552         if test "$usb_redir" = "yes"; then
4553             feature_not_found "usb-redir" "Install usbredir devel"
4554         fi
4555         usb_redir="no"
4556     fi
4557 fi
4558
4559 ##########################################
4560 # check if we have VSS SDK headers for win
4561
4562 if test "$mingw32" = "yes" && test "$guest_agent" != "no" && \
4563         test "$vss_win32_sdk" != "no" ; then
4564   case "$vss_win32_sdk" in
4565     "")   vss_win32_include="-isystem $source_path" ;;
4566     *\ *) # The SDK is installed in "Program Files" by default, but we cannot
4567           # handle path with spaces. So we symlink the headers into ".sdk/vss".
4568           vss_win32_include="-isystem $source_path/.sdk/vss"
4569           symlink "$vss_win32_sdk/inc" "$source_path/.sdk/vss/inc"
4570           ;;
4571     *)    vss_win32_include="-isystem $vss_win32_sdk"
4572   esac
4573   cat > $TMPC << EOF
4574 #define __MIDL_user_allocate_free_DEFINED__
4575 #include <inc/win2003/vss.h>
4576 int main(void) { return VSS_CTX_BACKUP; }
4577 EOF
4578   if compile_prog "$vss_win32_include" "" ; then
4579     guest_agent_with_vss="yes"
4580     QEMU_CFLAGS="$QEMU_CFLAGS $vss_win32_include"
4581     libs_qga="-lole32 -loleaut32 -lshlwapi -lstdc++ -Wl,--enable-stdcall-fixup $libs_qga"
4582     qga_vss_provider="qga/vss-win32/qga-vss.dll qga/vss-win32/qga-vss.tlb"
4583   else
4584     if test "$vss_win32_sdk" != "" ; then
4585       echo "ERROR: Please download and install Microsoft VSS SDK:"
4586       echo "ERROR:   http://www.microsoft.com/en-us/download/details.aspx?id=23490"
4587       echo "ERROR: On POSIX-systems, you can extract the SDK headers by:"
4588       echo "ERROR:   scripts/extract-vsssdk-headers setup.exe"
4589       echo "ERROR: The headers are extracted in the directory \`inc'."
4590       feature_not_found "VSS support"
4591     fi
4592     guest_agent_with_vss="no"
4593   fi
4594 fi
4595
4596 ##########################################
4597 # lookup Windows platform SDK (if not specified)
4598 # The SDK is needed only to build .tlb (type library) file of guest agent
4599 # VSS provider from the source. It is usually unnecessary because the
4600 # pre-compiled .tlb file is included.
4601
4602 if test "$mingw32" = "yes" && test "$guest_agent" != "no" && \
4603         test "$guest_agent_with_vss" = "yes" ; then
4604   if test -z "$win_sdk"; then
4605     programfiles="$PROGRAMFILES"
4606     test -n "$PROGRAMW6432" && programfiles="$PROGRAMW6432"
4607     if test -n "$programfiles"; then
4608       win_sdk=$(ls -d "$programfiles/Microsoft SDKs/Windows/v"* | tail -1) 2>/dev/null
4609     else
4610       feature_not_found "Windows SDK"
4611     fi
4612   elif test "$win_sdk" = "no"; then
4613     win_sdk=""
4614   fi
4615 fi
4616
4617 ##########################################
4618 # check if mingw environment provides a recent ntddscsi.h
4619 if test "$mingw32" = "yes" && test "$guest_agent" != "no"; then
4620   cat > $TMPC << EOF
4621 #include <windows.h>
4622 #include <ntddscsi.h>
4623 int main(void) {
4624 #if !defined(IOCTL_SCSI_GET_ADDRESS)
4625 #error Missing required ioctl definitions
4626 #endif
4627   SCSI_ADDRESS addr = { .Lun = 0, .TargetId = 0, .PathId = 0 };
4628   return addr.Lun;
4629 }
4630 EOF
4631   if compile_prog "" "" ; then
4632     guest_agent_ntddscsi=yes
4633     libs_qga="-lsetupapi -lcfgmgr32 $libs_qga"
4634   fi
4635 fi
4636
4637 ##########################################
4638 # virgl renderer probe
4639
4640 if test "$virglrenderer" != "no" ; then
4641   cat > $TMPC << EOF
4642 #include <virglrenderer.h>
4643 int main(void) { virgl_renderer_poll(); return 0; }
4644 EOF
4645   virgl_cflags=$($pkg_config --cflags virglrenderer 2>/dev/null)
4646   virgl_libs=$($pkg_config --libs virglrenderer 2>/dev/null)
4647   virgl_version=$($pkg_config --modversion virglrenderer 2>/dev/null)
4648   if $pkg_config virglrenderer >/dev/null 2>&1 && \
4649      compile_prog "$virgl_cflags" "$virgl_libs" ; then
4650     virglrenderer="yes"
4651   else
4652     if test "$virglrenderer" = "yes" ; then
4653       feature_not_found "virglrenderer"
4654     fi
4655     virglrenderer="no"
4656   fi
4657 fi
4658
4659 ##########################################
4660 # capstone
4661
4662 case "$capstone" in
4663   auto | enabled | internal)
4664     # Simpler to always update submodule, even if not needed.
4665     if test -e "${source_path}/.git" && test $git_update = 'yes' ; then
4666       git_submodules="${git_submodules} capstone"
4667     fi
4668     ;;
4669 esac
4670
4671 ##########################################
4672 # check if we have fdatasync
4673
4674 fdatasync=no
4675 cat > $TMPC << EOF
4676 #include <unistd.h>
4677 int main(void) {
4678 #if defined(_POSIX_SYNCHRONIZED_IO) && _POSIX_SYNCHRONIZED_IO > 0
4679 return fdatasync(0);
4680 #else
4681 #error Not supported
4682 #endif
4683 }
4684 EOF
4685 if compile_prog "" "" ; then
4686     fdatasync=yes
4687 fi
4688
4689 ##########################################
4690 # check if we have madvise
4691
4692 madvise=no
4693 cat > $TMPC << EOF
4694 #include <sys/types.h>
4695 #include <sys/mman.h>
4696 #include <stddef.h>
4697 int main(void) { return madvise(NULL, 0, MADV_DONTNEED); }
4698 EOF
4699 if compile_prog "" "" ; then
4700     madvise=yes
4701 fi
4702
4703 ##########################################
4704 # check if we have posix_madvise
4705
4706 posix_madvise=no
4707 cat > $TMPC << EOF
4708 #include <sys/mman.h>
4709 #include <stddef.h>
4710 int main(void) { return posix_madvise(NULL, 0, POSIX_MADV_DONTNEED); }
4711 EOF
4712 if compile_prog "" "" ; then
4713     posix_madvise=yes
4714 fi
4715
4716 ##########################################
4717 # check if we have posix_memalign()
4718
4719 posix_memalign=no
4720 cat > $TMPC << EOF
4721 #include <stdlib.h>
4722 int main(void) {
4723     void *p;
4724     return posix_memalign(&p, 8, 8);
4725 }
4726 EOF
4727 if compile_prog "" "" ; then
4728     posix_memalign=yes
4729 fi
4730
4731 ##########################################
4732 # check if we have posix_syslog
4733
4734 posix_syslog=no
4735 cat > $TMPC << EOF
4736 #include <syslog.h>
4737 int main(void) { openlog("qemu", LOG_PID, LOG_DAEMON); syslog(LOG_INFO, "configure"); return 0; }
4738 EOF
4739 if compile_prog "" "" ; then
4740     posix_syslog=yes
4741 fi
4742
4743 ##########################################
4744 # check if we have sem_timedwait
4745
4746 sem_timedwait=no
4747 cat > $TMPC << EOF
4748 #include <semaphore.h>
4749 int main(void) { sem_t s; struct timespec t = {0}; return sem_timedwait(&s, &t); }
4750 EOF
4751 if compile_prog "" "" ; then
4752     sem_timedwait=yes
4753 fi
4754
4755 ##########################################
4756 # check if we have strchrnul
4757
4758 strchrnul=no
4759 cat > $TMPC << EOF
4760 #include <string.h>
4761 int main(void);
4762 // Use a haystack that the compiler shouldn't be able to constant fold
4763 char *haystack = (char*)&main;
4764 int main(void) { return strchrnul(haystack, 'x') != &haystack[6]; }
4765 EOF
4766 if compile_prog "" "" ; then
4767     strchrnul=yes
4768 fi
4769
4770 #########################################
4771 # check if we have st_atim
4772
4773 st_atim=no
4774 cat > $TMPC << EOF
4775 #include <sys/stat.h>
4776 #include <stddef.h>
4777 int main(void) { return offsetof(struct stat, st_atim); }
4778 EOF
4779 if compile_prog "" "" ; then
4780     st_atim=yes
4781 fi
4782
4783 ##########################################
4784 # check if trace backend exists
4785
4786 $python "$source_path/scripts/tracetool.py" "--backends=$trace_backends" --check-backends  > /dev/null 2> /dev/null
4787 if test "$?" -ne 0 ; then
4788   error_exit "invalid trace backends" \
4789       "Please choose supported trace backends."
4790 fi
4791
4792 ##########################################
4793 # For 'ust' backend, test if ust headers are present
4794 if have_backend "ust"; then
4795   cat > $TMPC << EOF
4796 #include <lttng/tracepoint.h>
4797 int main(void) { return 0; }
4798 EOF
4799   if compile_prog "" "-Wl,--no-as-needed -ldl" ; then
4800     if $pkg_config lttng-ust --exists; then
4801       lttng_ust_libs=$($pkg_config --libs lttng-ust)
4802     else
4803       lttng_ust_libs="-llttng-ust -ldl"
4804     fi
4805     if $pkg_config liburcu-bp --exists; then
4806       urcu_bp_libs=$($pkg_config --libs liburcu-bp)
4807     else
4808       urcu_bp_libs="-lurcu-bp"
4809     fi
4810   else
4811     error_exit "Trace backend 'ust' missing lttng-ust header files"
4812   fi
4813 fi
4814
4815 ##########################################
4816 # For 'dtrace' backend, test if 'dtrace' command is present
4817 if have_backend "dtrace"; then
4818   if ! has 'dtrace' ; then
4819     error_exit "dtrace command is not found in PATH $PATH"
4820   fi
4821   trace_backend_stap="no"
4822   if has 'stap' ; then
4823     trace_backend_stap="yes"
4824
4825     # Workaround to avoid dtrace(1) producing a file with 'hidden' symbol
4826     # visibility. Define STAP_SDT_V2 to produce 'default' symbol visibility
4827     # instead. QEMU --enable-modules depends on this because the SystemTap
4828     # semaphores are linked into the main binary and not the module's shared
4829     # object.
4830     QEMU_CFLAGS="$QEMU_CFLAGS -DSTAP_SDT_V2"
4831   fi
4832 fi
4833
4834 ##########################################
4835 # check and set a backend for coroutine
4836
4837 # We prefer ucontext, but it's not always possible. The fallback
4838 # is sigcontext. On Windows the only valid backend is the Windows
4839 # specific one.
4840
4841 ucontext_works=no
4842 if test "$darwin" != "yes"; then
4843   cat > $TMPC << EOF
4844 #include <ucontext.h>
4845 #ifdef __stub_makecontext
4846 #error Ignoring glibc stub makecontext which will always fail
4847 #endif
4848 int main(void) { makecontext(0, 0, 0); return 0; }
4849 EOF
4850   if compile_prog "" "" ; then
4851     ucontext_works=yes
4852   fi
4853 fi
4854
4855 if test "$coroutine" = ""; then
4856   if test "$mingw32" = "yes"; then
4857     coroutine=win32
4858   elif test "$ucontext_works" = "yes"; then
4859     coroutine=ucontext
4860   else
4861     coroutine=sigaltstack
4862   fi
4863 else
4864   case $coroutine in
4865   windows)
4866     if test "$mingw32" != "yes"; then
4867       error_exit "'windows' coroutine backend only valid for Windows"
4868     fi
4869     # Unfortunately the user visible backend name doesn't match the
4870     # coroutine-*.c filename for this case, so we have to adjust it here.
4871     coroutine=win32
4872     ;;
4873   ucontext)
4874     if test "$ucontext_works" != "yes"; then
4875       feature_not_found "ucontext"
4876     fi
4877     ;;
4878   sigaltstack)
4879     if test "$mingw32" = "yes"; then
4880       error_exit "only the 'windows' coroutine backend is valid for Windows"
4881     fi
4882     ;;
4883   *)
4884     error_exit "unknown coroutine backend $coroutine"
4885     ;;
4886   esac
4887 fi
4888
4889 if test "$coroutine_pool" = ""; then
4890   coroutine_pool=yes
4891 fi
4892
4893 if test "$debug_stack_usage" = "yes"; then
4894   if test "$coroutine_pool" = "yes"; then
4895     echo "WARN: disabling coroutine pool for stack usage debugging"
4896     coroutine_pool=no
4897   fi
4898 fi
4899
4900 ##################################################
4901 # SafeStack
4902
4903
4904 if test "$safe_stack" = "yes"; then
4905 cat > $TMPC << EOF
4906 int main(int argc, char *argv[])
4907 {
4908 #if ! __has_feature(safe_stack)
4909 #error SafeStack Disabled
4910 #endif
4911     return 0;
4912 }
4913 EOF
4914   flag="-fsanitize=safe-stack"
4915   # Check that safe-stack is supported and enabled.
4916   if compile_prog "-Werror $flag" "$flag"; then
4917     # Flag needed both at compilation and at linking
4918     QEMU_CFLAGS="$QEMU_CFLAGS $flag"
4919     QEMU_LDFLAGS="$QEMU_LDFLAGS $flag"
4920   else
4921     error_exit "SafeStack not supported by your compiler"
4922   fi
4923   if test "$coroutine" != "ucontext"; then
4924     error_exit "SafeStack is only supported by the coroutine backend ucontext"
4925   fi
4926 else
4927 cat > $TMPC << EOF
4928 int main(int argc, char *argv[])
4929 {
4930 #if defined(__has_feature)
4931 #if __has_feature(safe_stack)
4932 #error SafeStack Enabled
4933 #endif
4934 #endif
4935     return 0;
4936 }
4937 EOF
4938 if test "$safe_stack" = "no"; then
4939   # Make sure that safe-stack is disabled
4940   if ! compile_prog "-Werror" ""; then
4941     # SafeStack was already enabled, try to explicitly remove the feature
4942     flag="-fno-sanitize=safe-stack"
4943     if ! compile_prog "-Werror $flag" "$flag"; then
4944       error_exit "Configure cannot disable SafeStack"
4945     fi
4946     QEMU_CFLAGS="$QEMU_CFLAGS $flag"
4947     QEMU_LDFLAGS="$QEMU_LDFLAGS $flag"
4948   fi
4949 else # "$safe_stack" = ""
4950   # Set safe_stack to yes or no based on pre-existing flags
4951   if compile_prog "-Werror" ""; then
4952     safe_stack="no"
4953   else
4954     safe_stack="yes"
4955     if test "$coroutine" != "ucontext"; then
4956       error_exit "SafeStack is only supported by the coroutine backend ucontext"
4957     fi
4958   fi
4959 fi
4960 fi
4961
4962 ##########################################
4963 # check if we have open_by_handle_at
4964
4965 open_by_handle_at=no
4966 cat > $TMPC << EOF
4967 #include <fcntl.h>
4968 #if !defined(AT_EMPTY_PATH)
4969 # error missing definition
4970 #else
4971 int main(void) { struct file_handle fh; return open_by_handle_at(0, &fh, 0); }
4972 #endif
4973 EOF
4974 if compile_prog "" "" ; then
4975     open_by_handle_at=yes
4976 fi
4977
4978 ########################################
4979 # check if we have linux/magic.h
4980
4981 linux_magic_h=no
4982 cat > $TMPC << EOF
4983 #include <linux/magic.h>
4984 int main(void) {
4985   return 0;
4986 }
4987 EOF
4988 if compile_prog "" "" ; then
4989     linux_magic_h=yes
4990 fi
4991
4992 ########################################
4993 # check if we have valgrind/valgrind.h
4994
4995 valgrind_h=no
4996 cat > $TMPC << EOF
4997 #include <valgrind/valgrind.h>
4998 int main(void) {
4999   return 0;
5000 }
5001 EOF
5002 if compile_prog "" "" ; then
5003     valgrind_h=yes
5004 fi
5005
5006 ########################################
5007 # check if environ is declared
5008
5009 has_environ=no
5010 cat > $TMPC << EOF
5011 #include <unistd.h>
5012 int main(void) {
5013     environ = 0;
5014     return 0;
5015 }
5016 EOF
5017 if compile_prog "" "" ; then
5018     has_environ=yes
5019 fi
5020
5021 ########################################
5022 # check if cpuid.h is usable.
5023
5024 cat > $TMPC << EOF
5025 #include <cpuid.h>
5026 int main(void) {
5027     unsigned a, b, c, d;
5028     int max = __get_cpuid_max(0, 0);
5029
5030     if (max >= 1) {
5031         __cpuid(1, a, b, c, d);
5032     }
5033
5034     if (max >= 7) {
5035         __cpuid_count(7, 0, a, b, c, d);
5036     }
5037
5038     return 0;
5039 }
5040 EOF
5041 if compile_prog "" "" ; then
5042     cpuid_h=yes
5043 fi
5044
5045 ##########################################
5046 # avx2 optimization requirement check
5047 #
5048 # There is no point enabling this if cpuid.h is not usable,
5049 # since we won't be able to select the new routines.
5050
5051 if test "$cpuid_h" = "yes" && test "$avx2_opt" != "no"; then
5052   cat > $TMPC << EOF
5053 #pragma GCC push_options
5054 #pragma GCC target("avx2")
5055 #include <cpuid.h>
5056 #include <immintrin.h>
5057 static int bar(void *a) {
5058     __m256i x = *(__m256i *)a;
5059     return _mm256_testz_si256(x, x);
5060 }
5061 int main(int argc, char *argv[]) { return bar(argv[0]); }
5062 EOF
5063   if compile_object "" ; then
5064     avx2_opt="yes"
5065   else
5066     avx2_opt="no"
5067   fi
5068 fi
5069
5070 ##########################################
5071 # avx512f optimization requirement check
5072 #
5073 # There is no point enabling this if cpuid.h is not usable,
5074 # since we won't be able to select the new routines.
5075 # by default, it is turned off.
5076 # if user explicitly want to enable it, check environment
5077
5078 if test "$cpuid_h" = "yes" && test "$avx512f_opt" = "yes"; then
5079   cat > $TMPC << EOF
5080 #pragma GCC push_options
5081 #pragma GCC target("avx512f")
5082 #include <cpuid.h>
5083 #include <immintrin.h>
5084 static int bar(void *a) {
5085     __m512i x = *(__m512i *)a;
5086     return _mm512_test_epi64_mask(x, x);
5087 }
5088 int main(int argc, char *argv[])
5089 {
5090         return bar(argv[0]);
5091 }
5092 EOF
5093   if ! compile_object "" ; then
5094     avx512f_opt="no"
5095   fi
5096 else
5097   avx512f_opt="no"
5098 fi
5099
5100 ########################################
5101 # check if __[u]int128_t is usable.
5102
5103 int128=no
5104 cat > $TMPC << EOF
5105 __int128_t a;
5106 __uint128_t b;
5107 int main (void) {
5108   a = a + b;
5109   b = a * b;
5110   a = a * a;
5111   return 0;
5112 }
5113 EOF
5114 if compile_prog "" "" ; then
5115     int128=yes
5116 fi
5117
5118 #########################################
5119 # See if 128-bit atomic operations are supported.
5120
5121 atomic128=no
5122 if test "$int128" = "yes"; then
5123   cat > $TMPC << EOF
5124 int main(void)
5125 {
5126   unsigned __int128 x = 0, y = 0;
5127   y = __atomic_load_16(&x, 0);
5128   __atomic_store_16(&x, y, 0);
5129   __atomic_compare_exchange_16(&x, &y, x, 0, 0, 0);
5130   return 0;
5131 }
5132 EOF
5133   if compile_prog "" "" ; then
5134     atomic128=yes
5135   fi
5136 fi
5137
5138 cmpxchg128=no
5139 if test "$int128" = yes && test "$atomic128" = no; then
5140   cat > $TMPC << EOF
5141 int main(void)
5142 {
5143   unsigned __int128 x = 0, y = 0;
5144   __sync_val_compare_and_swap_16(&x, y, x);
5145   return 0;
5146 }
5147 EOF
5148   if compile_prog "" "" ; then
5149     cmpxchg128=yes
5150   fi
5151 fi
5152
5153 #########################################
5154 # See if 64-bit atomic operations are supported.
5155 # Note that without __atomic builtins, we can only
5156 # assume atomic loads/stores max at pointer size.
5157
5158 cat > $TMPC << EOF
5159 #include <stdint.h>
5160 int main(void)
5161 {
5162   uint64_t x = 0, y = 0;
5163 #ifdef __ATOMIC_RELAXED
5164   y = __atomic_load_n(&x, __ATOMIC_RELAXED);
5165   __atomic_store_n(&x, y, __ATOMIC_RELAXED);
5166   __atomic_compare_exchange_n(&x, &y, x, 0, __ATOMIC_RELAXED, __ATOMIC_RELAXED);
5167   __atomic_exchange_n(&x, y, __ATOMIC_RELAXED);
5168   __atomic_fetch_add(&x, y, __ATOMIC_RELAXED);
5169 #else
5170   typedef char is_host64[sizeof(void *) >= sizeof(uint64_t) ? 1 : -1];
5171   __sync_lock_test_and_set(&x, y);
5172   __sync_val_compare_and_swap(&x, y, 0);
5173   __sync_fetch_and_add(&x, y);
5174 #endif
5175   return 0;
5176 }
5177 EOF
5178 if compile_prog "" "" ; then
5179   atomic64=yes
5180 fi
5181
5182 #########################################
5183 # See if --dynamic-list is supported by the linker
5184 ld_dynamic_list="no"
5185 if test "$static" = "no" ; then
5186     cat > $TMPTXT <<EOF
5187 {
5188   foo;
5189 };
5190 EOF
5191
5192     cat > $TMPC <<EOF
5193 #include <stdio.h>
5194 void foo(void);
5195
5196 void foo(void)
5197 {
5198   printf("foo\n");
5199 }
5200
5201 int main(void)
5202 {
5203   foo();
5204   return 0;
5205 }
5206 EOF
5207
5208     if compile_prog "" "-Wl,--dynamic-list=$TMPTXT" ; then
5209         ld_dynamic_list="yes"
5210     fi
5211 fi
5212
5213 #########################################
5214 # See if -exported_symbols_list is supported by the linker
5215
5216 ld_exported_symbols_list="no"
5217 if test "$static" = "no" ; then
5218     cat > $TMPTXT <<EOF
5219   _foo
5220 EOF
5221
5222     if compile_prog "" "-Wl,-exported_symbols_list,$TMPTXT" ; then
5223         ld_exported_symbols_list="yes"
5224     fi
5225 fi
5226
5227 if  test "$plugins" = "yes" &&
5228     test "$ld_dynamic_list" = "no" &&
5229     test "$ld_exported_symbols_list" = "no" ; then
5230   error_exit \
5231       "Plugin support requires dynamic linking and specifying a set of symbols " \
5232       "that are exported to plugins. Unfortunately your linker doesn't " \
5233       "support the flag (--dynamic-list or -exported_symbols_list) used " \
5234       "for this purpose. You can't build with --static."
5235 fi
5236
5237 ########################################
5238 # See if __attribute__((alias)) is supported.
5239 # This false for Xcode 9, but has been remedied for Xcode 10.
5240 # Unfortunately, travis uses Xcode 9 by default.
5241
5242 attralias=no
5243 cat > $TMPC << EOF
5244 int x = 1;
5245 extern const int y __attribute__((alias("x")));
5246 int main(void) { return 0; }
5247 EOF
5248 if compile_prog "" "" ; then
5249     attralias=yes
5250 fi
5251
5252 ########################################
5253 # check if getauxval is available.
5254
5255 getauxval=no
5256 cat > $TMPC << EOF
5257 #include <sys/auxv.h>
5258 int main(void) {
5259   return getauxval(AT_HWCAP) == 0;
5260 }
5261 EOF
5262 if compile_prog "" "" ; then
5263     getauxval=yes
5264 fi
5265
5266 ########################################
5267 # check if ccache is interfering with
5268 # semantic analysis of macros
5269
5270 unset CCACHE_CPP2
5271 ccache_cpp2=no
5272 cat > $TMPC << EOF
5273 static const int Z = 1;
5274 #define fn() ({ Z; })
5275 #define TAUT(X) ((X) == Z)
5276 #define PAREN(X, Y) (X == Y)
5277 #define ID(X) (X)
5278 int main(int argc, char *argv[])
5279 {
5280     int x = 0, y = 0;
5281     x = ID(x);
5282     x = fn();
5283     fn();
5284     if (PAREN(x, y)) return 0;
5285     if (TAUT(Z)) return 0;
5286     return 0;
5287 }
5288 EOF
5289
5290 if ! compile_object "-Werror"; then
5291     ccache_cpp2=yes
5292 fi
5293
5294 #################################################
5295 # clang does not support glibc + FORTIFY_SOURCE.
5296
5297 if test "$fortify_source" != "no"; then
5298   if echo | $cc -dM -E - | grep __clang__ > /dev/null 2>&1 ; then
5299     fortify_source="no";
5300   elif test -n "$cxx" && has $cxx &&
5301        echo | $cxx -dM -E - | grep __clang__ >/dev/null 2>&1 ; then
5302     fortify_source="no";
5303   else
5304     fortify_source="yes"
5305   fi
5306 fi
5307
5308 ###############################################
5309 # Check if copy_file_range is provided by glibc
5310 have_copy_file_range=no
5311 cat > $TMPC << EOF
5312 #include <unistd.h>
5313 int main(void) {
5314   copy_file_range(0, NULL, 0, NULL, 0, 0);
5315   return 0;
5316 }
5317 EOF
5318 if compile_prog "" "" ; then
5319     have_copy_file_range=yes
5320 fi
5321
5322 ##########################################
5323 # check if struct fsxattr is available via linux/fs.h
5324
5325 have_fsxattr=no
5326 cat > $TMPC << EOF
5327 #include <linux/fs.h>
5328 struct fsxattr foo;
5329 int main(void) {
5330   return 0;
5331 }
5332 EOF
5333 if compile_prog "" "" ; then
5334     have_fsxattr=yes
5335 fi
5336
5337 ##########################################
5338 # check for usable membarrier system call
5339 if test "$membarrier" = "yes"; then
5340     have_membarrier=no
5341     if test "$mingw32" = "yes" ; then
5342         have_membarrier=yes
5343     elif test "$linux" = "yes" ; then
5344         cat > $TMPC << EOF
5345     #include <linux/membarrier.h>
5346     #include <sys/syscall.h>
5347     #include <unistd.h>
5348     #include <stdlib.h>
5349     int main(void) {
5350         syscall(__NR_membarrier, MEMBARRIER_CMD_QUERY, 0);
5351         syscall(__NR_membarrier, MEMBARRIER_CMD_SHARED, 0);
5352         exit(0);
5353     }
5354 EOF
5355         if compile_prog "" "" ; then
5356             have_membarrier=yes
5357         fi
5358     fi
5359     if test "$have_membarrier" = "no"; then
5360       feature_not_found "membarrier" "membarrier system call not available"
5361     fi
5362 else
5363     # Do not enable it by default even for Mingw32, because it doesn't
5364     # work on Wine.
5365     membarrier=no
5366 fi
5367
5368 ##########################################
5369 # check if rtnetlink.h exists and is useful
5370 have_rtnetlink=no
5371 cat > $TMPC << EOF
5372 #include <linux/rtnetlink.h>
5373 int main(void) {
5374   return IFLA_PROTO_DOWN;
5375 }
5376 EOF
5377 if compile_prog "" "" ; then
5378     have_rtnetlink=yes
5379 fi
5380
5381 ##########################################
5382 # check for usable AF_VSOCK environment
5383 have_af_vsock=no
5384 cat > $TMPC << EOF
5385 #include <errno.h>
5386 #include <sys/types.h>
5387 #include <sys/socket.h>
5388 #if !defined(AF_VSOCK)
5389 # error missing AF_VSOCK flag
5390 #endif
5391 #include <linux/vm_sockets.h>
5392 int main(void) {
5393     int sock, ret;
5394     struct sockaddr_vm svm;
5395     socklen_t len = sizeof(svm);
5396     sock = socket(AF_VSOCK, SOCK_STREAM, 0);
5397     ret = getpeername(sock, (struct sockaddr *)&svm, &len);
5398     if ((ret == -1) && (errno == ENOTCONN)) {
5399         return 0;
5400     }
5401     return -1;
5402 }
5403 EOF
5404 if compile_prog "" "" ; then
5405     have_af_vsock=yes
5406 fi
5407
5408 ##########################################
5409 # check for usable AF_ALG environment
5410 have_afalg=no
5411 cat > $TMPC << EOF
5412 #include <errno.h>
5413 #include <sys/types.h>
5414 #include <sys/socket.h>
5415 #include <linux/if_alg.h>
5416 int main(void) {
5417     int sock;
5418     sock = socket(AF_ALG, SOCK_SEQPACKET, 0);
5419     return sock;
5420 }
5421 EOF
5422 if compile_prog "" "" ; then
5423     have_afalg=yes
5424 fi
5425 if test "$crypto_afalg" = "yes"
5426 then
5427     if test "$have_afalg" != "yes"
5428     then
5429         error_exit "AF_ALG requested but could not be detected"
5430     fi
5431 fi
5432
5433
5434 #################################################
5435 # check for sysmacros.h
5436
5437 have_sysmacros=no
5438 cat > $TMPC << EOF
5439 #include <sys/sysmacros.h>
5440 int main(void) {
5441     return makedev(0, 0);
5442 }
5443 EOF
5444 if compile_prog "" "" ; then
5445     have_sysmacros=yes
5446 fi
5447
5448 ##########################################
5449 # check for _Static_assert()
5450
5451 have_static_assert=no
5452 cat > $TMPC << EOF
5453 _Static_assert(1, "success");
5454 int main(void) {
5455     return 0;
5456 }
5457 EOF
5458 if compile_prog "" "" ; then
5459     have_static_assert=yes
5460 fi
5461
5462 ##########################################
5463 # check for utmpx.h, it is missing e.g. on OpenBSD
5464
5465 have_utmpx=no
5466 cat > $TMPC << EOF
5467 #include <utmpx.h>
5468 struct utmpx user_info;
5469 int main(void) {
5470     return 0;
5471 }
5472 EOF
5473 if compile_prog "" "" ; then
5474     have_utmpx=yes
5475 fi
5476
5477 ##########################################
5478 # check for getrandom()
5479
5480 have_getrandom=no
5481 cat > $TMPC << EOF
5482 #include <sys/random.h>
5483 int main(void) {
5484     return getrandom(0, 0, GRND_NONBLOCK);
5485 }
5486 EOF
5487 if compile_prog "" "" ; then
5488     have_getrandom=yes
5489 fi
5490
5491 ##########################################
5492 # checks for sanitizers
5493
5494 have_asan=no
5495 have_ubsan=no
5496 have_asan_iface_h=no
5497 have_asan_iface_fiber=no
5498
5499 if test "$sanitizers" = "yes" ; then
5500   write_c_skeleton
5501   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=address" ""; then
5502       have_asan=yes
5503   fi
5504
5505   # we could use a simple skeleton for flags checks, but this also
5506   # detect the static linking issue of ubsan, see also:
5507   # https://gcc.gnu.org/bugzilla/show_bug.cgi?id=84285
5508   cat > $TMPC << EOF
5509 #include <stdlib.h>
5510 int main(void) {
5511     void *tmp = malloc(10);
5512     if (tmp != NULL) {
5513         return *(int *)(tmp + 2);
5514     }
5515     return 1;
5516 }
5517 EOF
5518   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=undefined" ""; then
5519       have_ubsan=yes
5520   fi
5521
5522   if check_include "sanitizer/asan_interface.h" ; then
5523       have_asan_iface_h=yes
5524   fi
5525
5526   cat > $TMPC << EOF
5527 #include <sanitizer/asan_interface.h>
5528 int main(void) {
5529   __sanitizer_start_switch_fiber(0, 0, 0);
5530   return 0;
5531 }
5532 EOF
5533   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=address" "" ; then
5534       have_asan_iface_fiber=yes
5535   fi
5536 fi
5537
5538 ##########################################
5539 # checks for fuzzer
5540 if test "$fuzzing" = "yes" && test -z "${LIB_FUZZING_ENGINE+xxx}"; then
5541   write_c_fuzzer_skeleton
5542   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=fuzzer" ""; then
5543     have_fuzzer=yes
5544   else
5545     error_exit "Your compiler doesn't support -fsanitize=fuzzer"
5546     exit 1
5547   fi
5548 fi
5549
5550 # Thread sanitizer is, for now, much noisier than the other sanitizers;
5551 # keep it separate until that is not the case.
5552 if test "$tsan" = "yes" && test "$sanitizers" = "yes"; then
5553   error_exit "TSAN is not supported with other sanitiziers."
5554 fi
5555 have_tsan=no
5556 have_tsan_iface_fiber=no
5557 if test "$tsan" = "yes" ; then
5558   write_c_skeleton
5559   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=thread" "" ; then
5560       have_tsan=yes
5561   fi
5562   cat > $TMPC << EOF
5563 #include <sanitizer/tsan_interface.h>
5564 int main(void) {
5565   __tsan_create_fiber(0);
5566   return 0;
5567 }
5568 EOF
5569   if compile_prog "$CPU_CFLAGS -Werror -fsanitize=thread" "" ; then
5570       have_tsan_iface_fiber=yes
5571   fi
5572 fi
5573
5574 ##########################################
5575 # check for libpmem
5576
5577 if test "$libpmem" != "no"; then
5578         if $pkg_config --exists "libpmem"; then
5579                 libpmem="yes"
5580                 libpmem_libs=$($pkg_config --libs libpmem)
5581                 libpmem_cflags=$($pkg_config --cflags libpmem)
5582         else
5583                 if test "$libpmem" = "yes" ; then
5584                         feature_not_found "libpmem" "Install nvml or pmdk"
5585                 fi
5586                 libpmem="no"
5587         fi
5588 fi
5589
5590 ##########################################
5591 # check for libdaxctl
5592
5593 if test "$libdaxctl" != "no"; then
5594         if $pkg_config --atleast-version=57 "libdaxctl"; then
5595                 libdaxctl="yes"
5596                 libdaxctl_libs=$($pkg_config --libs libdaxctl)
5597                 libdaxctl_cflags=$($pkg_config --cflags libdaxctl)
5598         else
5599                 if test "$libdaxctl" = "yes" ; then
5600                         feature_not_found "libdaxctl" "Install libdaxctl"
5601                 fi
5602                 libdaxctl="no"
5603         fi
5604 fi
5605
5606 ##########################################
5607 # check for slirp
5608
5609 case "$slirp" in
5610   auto | enabled | internal)
5611     # Simpler to always update submodule, even if not needed.
5612     if test -e "${source_path}/.git" && test $git_update = 'yes' ; then
5613       git_submodules="${git_submodules} slirp"
5614     fi
5615     ;;
5616 esac
5617
5618 ##########################################
5619 # check for usable __NR_keyctl syscall
5620
5621 if test "$linux" = "yes" ; then
5622
5623     have_keyring=no
5624     cat > $TMPC << EOF
5625 #include <errno.h>
5626 #include <asm/unistd.h>
5627 #include <linux/keyctl.h>
5628 #include <unistd.h>
5629 int main(void) {
5630     return syscall(__NR_keyctl, KEYCTL_READ, 0, NULL, NULL, 0);
5631 }
5632 EOF
5633     if compile_prog "" "" ; then
5634         have_keyring=yes
5635     fi
5636 fi
5637 if test "$secret_keyring" != "no"
5638 then
5639     if test "$have_keyring" = "yes"
5640     then
5641         secret_keyring=yes
5642     else
5643         if test "$secret_keyring" = "yes"
5644         then
5645             error_exit "syscall __NR_keyctl requested, \
5646 but not implemented on your system"
5647         else
5648             secret_keyring=no
5649         fi
5650     fi
5651 fi
5652
5653 ##########################################
5654 # End of CC checks
5655 # After here, no more $cc or $ld runs
5656
5657 write_c_skeleton
5658
5659 if test "$gcov" = "yes" ; then
5660   :
5661 elif test "$fortify_source" = "yes" ; then
5662   QEMU_CFLAGS="-U_FORTIFY_SOURCE -D_FORTIFY_SOURCE=2 $QEMU_CFLAGS"
5663   debug=no
5664 fi
5665
5666 case "$ARCH" in
5667 alpha)
5668   # Ensure there's only a single GP
5669   QEMU_CFLAGS="-msmall-data $QEMU_CFLAGS"
5670 ;;
5671 esac
5672
5673 if test "$gprof" = "yes" ; then
5674   QEMU_CFLAGS="-p $QEMU_CFLAGS"
5675   QEMU_LDFLAGS="-p $QEMU_LDFLAGS"
5676 fi
5677
5678 if test "$have_asan" = "yes"; then
5679   QEMU_CFLAGS="-fsanitize=address $QEMU_CFLAGS"
5680   QEMU_LDFLAGS="-fsanitize=address $QEMU_LDFLAGS"
5681   if test "$have_asan_iface_h" = "no" ; then
5682       echo "ASAN build enabled, but ASAN header missing." \
5683            "Without code annotation, the report may be inferior."
5684   elif test "$have_asan_iface_fiber" = "no" ; then
5685       echo "ASAN build enabled, but ASAN header is too old." \
5686            "Without code annotation, the report may be inferior."
5687   fi
5688 fi
5689 if test "$have_tsan" = "yes" ; then
5690   if test "$have_tsan_iface_fiber" = "yes" ; then
5691     QEMU_CFLAGS="-fsanitize=thread $QEMU_CFLAGS"
5692     QEMU_LDFLAGS="-fsanitize=thread $QEMU_LDFLAGS"
5693   else
5694     error_exit "Cannot enable TSAN due to missing fiber annotation interface."
5695   fi
5696 elif test "$tsan" = "yes" ; then
5697   error_exit "Cannot enable TSAN due to missing sanitize thread interface."
5698 fi
5699 if test "$have_ubsan" = "yes"; then
5700   QEMU_CFLAGS="-fsanitize=undefined $QEMU_CFLAGS"
5701   QEMU_LDFLAGS="-fsanitize=undefined $QEMU_LDFLAGS"
5702 fi
5703
5704 ##########################################
5705 # Do we have libnfs
5706 if test "$libnfs" != "no" ; then
5707   if $pkg_config --atleast-version=1.9.3 libnfs; then
5708     libnfs="yes"
5709     libnfs_libs=$($pkg_config --libs libnfs)
5710   else
5711     if test "$libnfs" = "yes" ; then
5712       feature_not_found "libnfs" "Install libnfs devel >= 1.9.3"
5713     fi
5714     libnfs="no"
5715   fi
5716 fi
5717
5718 ##########################################
5719
5720 # Exclude --warn-common with TSan to suppress warnings from the TSan libraries.
5721 if test "$solaris" = "no" && test "$tsan" = "no"; then
5722     if $ld --version 2>/dev/null | grep "GNU ld" >/dev/null 2>/dev/null ; then
5723         QEMU_LDFLAGS="-Wl,--warn-common $QEMU_LDFLAGS"
5724     fi
5725 fi
5726
5727 # Use ASLR, no-SEH and DEP if available
5728 if test "$mingw32" = "yes" ; then
5729     flags="--no-seh --nxcompat"
5730
5731     # Disable ASLR for debug builds to allow debugging with gdb
5732     if test "$debug" = "no" ; then
5733         flags="--dynamicbase $flags"
5734     fi
5735
5736     for flag in $flags; do
5737         if ld_has $flag ; then
5738             QEMU_LDFLAGS="-Wl,$flag $QEMU_LDFLAGS"
5739         fi
5740     done
5741 fi
5742
5743 # We can only support ivshmem if we have eventfd
5744 if [ "$eventfd" = "yes" ]; then
5745   ivshmem=yes
5746 fi
5747
5748 if test "$softmmu" = yes ; then
5749   if test "$linux" = yes; then
5750     if test "$virtfs" != no && test "$cap_ng" = yes && test "$attr" = yes ; then
5751       virtfs=yes
5752     else
5753       if test "$virtfs" = yes; then
5754         error_exit "VirtFS requires libcap-ng devel and libattr devel"
5755       fi
5756       virtfs=no
5757     fi
5758   else
5759     if test "$virtfs" = yes; then
5760       error_exit "VirtFS is supported only on Linux"
5761     fi
5762     virtfs=no
5763   fi
5764 fi
5765
5766 # Probe for guest agent support/options
5767
5768 if [ "$guest_agent" != "no" ]; then
5769   if [ "$softmmu" = no -a "$want_tools" = no ] ; then
5770       guest_agent=no
5771   elif [ "$linux" = "yes" -o "$bsd" = "yes" -o "$solaris" = "yes" -o "$mingw32" = "yes" ] ; then
5772       guest_agent=yes
5773   elif [ "$guest_agent" != yes ]; then
5774       guest_agent=no
5775   else
5776       error_exit "Guest agent is not supported on this platform"
5777   fi
5778 fi
5779
5780 # Guest agent Window MSI  package
5781
5782 if test "$guest_agent" != yes; then
5783   if test "$guest_agent_msi" = yes; then
5784     error_exit "MSI guest agent package requires guest agent enabled"
5785   fi
5786   guest_agent_msi=no
5787 elif test "$mingw32" != "yes"; then
5788   if test "$guest_agent_msi" = "yes"; then
5789     error_exit "MSI guest agent package is available only for MinGW Windows cross-compilation"
5790   fi
5791   guest_agent_msi=no
5792 elif ! has wixl; then
5793   if test "$guest_agent_msi" = "yes"; then
5794     error_exit "MSI guest agent package requires wixl tool installed ( usually from msitools package )"
5795   fi
5796   guest_agent_msi=no
5797 else
5798   # we support qemu-ga, mingw32, and wixl: default to MSI enabled if it wasn't
5799   # disabled explicitly
5800   if test "$guest_agent_msi" != "no"; then
5801     guest_agent_msi=yes
5802   fi
5803 fi
5804
5805 if test "$guest_agent_msi" = "yes"; then
5806   if test "$guest_agent_with_vss" = "yes"; then
5807     QEMU_GA_MSI_WITH_VSS="-D InstallVss"
5808   fi
5809
5810   if test "$QEMU_GA_MANUFACTURER" = ""; then
5811     QEMU_GA_MANUFACTURER=QEMU
5812   fi
5813
5814   if test "$QEMU_GA_DISTRO" = ""; then
5815     QEMU_GA_DISTRO=Linux
5816   fi
5817
5818   if test "$QEMU_GA_VERSION" = ""; then
5819       QEMU_GA_VERSION=$(cat $source_path/VERSION)
5820   fi
5821
5822   QEMU_GA_MSI_MINGW_DLL_PATH="-D Mingw_dlls=$($pkg_config --variable=prefix glib-2.0)/bin"
5823
5824   case "$cpu" in
5825   x86_64)
5826     QEMU_GA_MSI_ARCH="-a x64 -D Arch=64"
5827     ;;
5828   i386)
5829     QEMU_GA_MSI_ARCH="-D Arch=32"
5830     ;;
5831   *)
5832     error_exit "CPU $cpu not supported for building installation package"
5833     ;;
5834   esac
5835 fi
5836
5837 # Mac OS X ships with a broken assembler
5838 roms=
5839 if { test "$cpu" = "i386" || test "$cpu" = "x86_64"; } && \
5840         test "$targetos" != "Darwin" && test "$targetos" != "SunOS" && \
5841         test "$targetos" != "Haiku" && test "$softmmu" = yes ; then
5842     # Different host OS linkers have different ideas about the name of the ELF
5843     # emulation. Linux and OpenBSD/amd64 use 'elf_i386'; FreeBSD uses the _fbsd
5844     # variant; OpenBSD/i386 uses the _obsd variant; and Windows uses i386pe.
5845     for emu in elf_i386 elf_i386_fbsd elf_i386_obsd i386pe; do
5846         if "$ld" -verbose 2>&1 | grep -q "^[[:space:]]*$emu[[:space:]]*$"; then
5847             ld_i386_emulation="$emu"
5848             roms="optionrom"
5849             break
5850         fi
5851     done
5852 fi
5853
5854 # Only build s390-ccw bios if we're on s390x and the compiler has -march=z900
5855 if test "$cpu" = "s390x" ; then
5856   write_c_skeleton
5857   if compile_prog "-march=z900" ""; then
5858     roms="$roms s390-ccw"
5859     # SLOF is required for building the s390-ccw firmware on s390x,
5860     # since it is using the libnet code from SLOF for network booting.
5861     if test -e "${source_path}/.git" ; then
5862       git_submodules="${git_submodules} roms/SLOF"
5863     fi
5864   fi
5865 fi
5866
5867 # Check that the C++ compiler exists and works with the C compiler.
5868 # All the QEMU_CXXFLAGS are based on QEMU_CFLAGS. Keep this at the end to don't miss any other that could be added.
5869 if has $cxx; then
5870     cat > $TMPC <<EOF
5871 int c_function(void);
5872 int main(void) { return c_function(); }
5873 EOF
5874
5875     compile_object
5876
5877     cat > $TMPCXX <<EOF
5878 extern "C" {
5879    int c_function(void);
5880 }
5881 int c_function(void) { return 42; }
5882 EOF
5883
5884     update_cxxflags
5885
5886     if do_cxx $CXXFLAGS $CONFIGURE_CXXFLAGS $QEMU_CXXFLAGS -o $TMPE $TMPCXX $TMPO $QEMU_LDFLAGS; then
5887         # C++ compiler $cxx works ok with C compiler $cc
5888         :
5889     else
5890         echo "C++ compiler $cxx does not work with C compiler $cc"
5891         echo "Disabling C++ specific optional code"
5892         cxx=
5893     fi
5894 else
5895     echo "No C++ compiler available; disabling C++ specific optional code"
5896     cxx=
5897 fi
5898
5899 if test $git_update = 'yes' ; then
5900     (cd "${source_path}" && GIT="$git" "./scripts/git-submodule.sh" update "$git_submodules")
5901 fi
5902
5903 config_host_mak="config-host.mak"
5904
5905 echo "# Automatically generated by configure - do not modify" > $config_host_mak
5906 echo >> $config_host_mak
5907
5908 echo all: >> $config_host_mak
5909 echo "GIT=$git" >> $config_host_mak
5910 echo "GIT_SUBMODULES=$git_submodules" >> $config_host_mak
5911 echo "GIT_UPDATE=$git_update" >> $config_host_mak
5912
5913 echo "ARCH=$ARCH" >> $config_host_mak
5914
5915 if test "$default_devices" = "yes" ; then
5916   echo "CONFIG_MINIKCONF_MODE=--defconfig" >> $config_host_mak
5917 else
5918   echo "CONFIG_MINIKCONF_MODE=--allnoconfig" >> $config_host_mak
5919 fi
5920 if test "$debug_tcg" = "yes" ; then
5921   echo "CONFIG_DEBUG_TCG=y" >> $config_host_mak
5922 fi
5923 if test "$strip_opt" = "yes" ; then
5924   echo "STRIP=${strip}" >> $config_host_mak
5925 fi
5926 if test "$bigendian" = "yes" ; then
5927   echo "HOST_WORDS_BIGENDIAN=y" >> $config_host_mak
5928 fi
5929 if test "$mingw32" = "yes" ; then
5930   echo "CONFIG_WIN32=y" >> $config_host_mak
5931   rc_version=$(cat $source_path/VERSION)
5932   version_major=${rc_version%%.*}
5933   rc_version=${rc_version#*.}
5934   version_minor=${rc_version%%.*}
5935   rc_version=${rc_version#*.}
5936   version_subminor=${rc_version%%.*}
5937   version_micro=0
5938   echo "CONFIG_FILEVERSION=$version_major,$version_minor,$version_subminor,$version_micro" >> $config_host_mak
5939   echo "CONFIG_PRODUCTVERSION=$version_major,$version_minor,$version_subminor,$version_micro" >> $config_host_mak
5940   if test "$guest_agent_with_vss" = "yes" ; then
5941     echo "CONFIG_QGA_VSS=y" >> $config_host_mak
5942     echo "QGA_VSS_PROVIDER=$qga_vss_provider" >> $config_host_mak
5943     echo "WIN_SDK=\"$win_sdk\"" >> $config_host_mak
5944   fi
5945   if test "$guest_agent_ntddscsi" = "yes" ; then
5946     echo "CONFIG_QGA_NTDDSCSI=y" >> $config_host_mak
5947   fi
5948   if test "$guest_agent_msi" = "yes"; then
5949     echo "CONFIG_QGA_MSI=y" >> $config_host_mak
5950     echo "QEMU_GA_MSI_MINGW_DLL_PATH=${QEMU_GA_MSI_MINGW_DLL_PATH}" >> $config_host_mak
5951     echo "QEMU_GA_MSI_WITH_VSS=${QEMU_GA_MSI_WITH_VSS}" >> $config_host_mak
5952     echo "QEMU_GA_MSI_ARCH=${QEMU_GA_MSI_ARCH}" >> $config_host_mak
5953     echo "QEMU_GA_MANUFACTURER=${QEMU_GA_MANUFACTURER}" >> $config_host_mak
5954     echo "QEMU_GA_DISTRO=${QEMU_GA_DISTRO}" >> $config_host_mak
5955     echo "QEMU_GA_VERSION=${QEMU_GA_VERSION}" >> $config_host_mak
5956   fi
5957 else
5958   echo "CONFIG_POSIX=y" >> $config_host_mak
5959 fi
5960
5961 if test "$linux" = "yes" ; then
5962   echo "CONFIG_LINUX=y" >> $config_host_mak
5963 fi
5964
5965 if test "$darwin" = "yes" ; then
5966   echo "CONFIG_DARWIN=y" >> $config_host_mak
5967 fi
5968
5969 if test "$solaris" = "yes" ; then
5970   echo "CONFIG_SOLARIS=y" >> $config_host_mak
5971 fi
5972 if test "$haiku" = "yes" ; then
5973   echo "CONFIG_HAIKU=y" >> $config_host_mak
5974 fi
5975 if test "$static" = "yes" ; then
5976   echo "CONFIG_STATIC=y" >> $config_host_mak
5977 fi
5978 if test "$profiler" = "yes" ; then
5979   echo "CONFIG_PROFILER=y" >> $config_host_mak
5980 fi
5981 if test "$want_tools" = "yes" ; then
5982   echo "CONFIG_TOOLS=y" >> $config_host_mak
5983 fi
5984 if test "$guest_agent" = "yes" ; then
5985   echo "CONFIG_GUEST_AGENT=y" >> $config_host_mak
5986 fi
5987 echo "CONFIG_SMBD_COMMAND=\"$smbd\"" >> $config_host_mak
5988 if test "$vde" = "yes" ; then
5989   echo "CONFIG_VDE=y" >> $config_host_mak
5990   echo "VDE_LIBS=$vde_libs" >> $config_host_mak
5991 fi
5992 if test "$netmap" = "yes" ; then
5993   echo "CONFIG_NETMAP=y" >> $config_host_mak
5994 fi
5995 if test "$l2tpv3" = "yes" ; then
5996   echo "CONFIG_L2TPV3=y" >> $config_host_mak
5997 fi
5998 if test "$gprof" = "yes" ; then
5999   echo "CONFIG_GPROF=y" >> $config_host_mak
6000 fi
6001 if test "$cap_ng" = "yes" ; then
6002   echo "CONFIG_LIBCAP_NG=y" >> $config_host_mak
6003   echo "LIBCAP_NG_LIBS=$cap_libs" >> $config_host_mak
6004 fi
6005 echo "CONFIG_AUDIO_DRIVERS=$audio_drv_list" >> $config_host_mak
6006 for drv in $audio_drv_list; do
6007     def=CONFIG_AUDIO_$(echo $drv | LC_ALL=C tr '[a-z]' '[A-Z]')
6008     echo "$def=y" >> $config_host_mak
6009 done
6010 if test "$alsa" = "yes" ; then
6011     echo "CONFIG_ALSA=y" >> $config_host_mak
6012 fi
6013 echo "ALSA_LIBS=$alsa_libs" >> $config_host_mak
6014 echo "ALSA_CFLAGS=$alsa_cflags" >> $config_host_mak
6015 if test "$libpulse" = "yes" ; then
6016     echo "CONFIG_LIBPULSE=y" >> $config_host_mak
6017 fi
6018 echo "PULSE_LIBS=$pulse_libs" >> $config_host_mak
6019 echo "PULSE_CFLAGS=$pulse_cflags" >> $config_host_mak
6020 echo "COREAUDIO_LIBS=$coreaudio_libs" >> $config_host_mak
6021 echo "DSOUND_LIBS=$dsound_libs" >> $config_host_mak
6022 echo "OSS_LIBS=$oss_libs" >> $config_host_mak
6023 if test "$libjack" = "yes" ; then
6024     echo "CONFIG_LIBJACK=y" >> $config_host_mak
6025 fi
6026 echo "JACK_LIBS=$jack_libs" >> $config_host_mak
6027 if test "$audio_win_int" = "yes" ; then
6028   echo "CONFIG_AUDIO_WIN_INT=y" >> $config_host_mak
6029 fi
6030 echo "CONFIG_BDRV_RW_WHITELIST=$block_drv_rw_whitelist" >> $config_host_mak
6031 echo "CONFIG_BDRV_RO_WHITELIST=$block_drv_ro_whitelist" >> $config_host_mak
6032 if test "$xfs" = "yes" ; then
6033   echo "CONFIG_XFS=y" >> $config_host_mak
6034 fi
6035 qemu_version=$(head $source_path/VERSION)
6036 echo "PKGVERSION=$pkgversion" >>$config_host_mak
6037 echo "SRC_PATH=$source_path" >> $config_host_mak
6038 echo "TARGET_DIRS=$target_list" >> $config_host_mak
6039 if test "$modules" = "yes"; then
6040   # $shacmd can generate a hash started with digit, which the compiler doesn't
6041   # like as an symbol. So prefix it with an underscore
6042   echo "CONFIG_STAMP=_$( (echo $qemu_version; echo $pkgversion; cat $0) | $shacmd - | cut -f1 -d\ )" >> $config_host_mak
6043   echo "CONFIG_MODULES=y" >> $config_host_mak
6044 fi
6045 if test "$module_upgrades" = "yes"; then
6046   echo "CONFIG_MODULE_UPGRADES=y" >> $config_host_mak
6047 fi
6048 if test "$have_x11" = "yes" && test "$need_x11" = "yes"; then
6049   echo "CONFIG_X11=y" >> $config_host_mak
6050   echo "X11_CFLAGS=$x11_cflags" >> $config_host_mak
6051   echo "X11_LIBS=$x11_libs" >> $config_host_mak
6052 fi
6053 if test "$pipe2" = "yes" ; then
6054   echo "CONFIG_PIPE2=y" >> $config_host_mak
6055 fi
6056 if test "$accept4" = "yes" ; then
6057   echo "CONFIG_ACCEPT4=y" >> $config_host_mak
6058 fi
6059 if test "$splice" = "yes" ; then
6060   echo "CONFIG_SPLICE=y" >> $config_host_mak
6061 fi
6062 if test "$eventfd" = "yes" ; then
6063   echo "CONFIG_EVENTFD=y" >> $config_host_mak
6064 fi
6065 if test "$memfd" = "yes" ; then
6066   echo "CONFIG_MEMFD=y" >> $config_host_mak
6067 fi
6068 if test "$have_usbfs" = "yes" ; then
6069   echo "CONFIG_USBFS=y" >> $config_host_mak
6070 fi
6071 if test "$fallocate" = "yes" ; then
6072   echo "CONFIG_FALLOCATE=y" >> $config_host_mak
6073 fi
6074 if test "$fallocate_punch_hole" = "yes" ; then
6075   echo "CONFIG_FALLOCATE_PUNCH_HOLE=y" >> $config_host_mak
6076 fi
6077 if test "$fallocate_zero_range" = "yes" ; then
6078   echo "CONFIG_FALLOCATE_ZERO_RANGE=y" >> $config_host_mak
6079 fi
6080 if test "$posix_fallocate" = "yes" ; then
6081   echo "CONFIG_POSIX_FALLOCATE=y" >> $config_host_mak
6082 fi
6083 if test "$sync_file_range" = "yes" ; then
6084   echo "CONFIG_SYNC_FILE_RANGE=y" >> $config_host_mak
6085 fi
6086 if test "$fiemap" = "yes" ; then
6087   echo "CONFIG_FIEMAP=y" >> $config_host_mak
6088 fi
6089 if test "$dup3" = "yes" ; then
6090   echo "CONFIG_DUP3=y" >> $config_host_mak
6091 fi
6092 if test "$ppoll" = "yes" ; then
6093   echo "CONFIG_PPOLL=y" >> $config_host_mak
6094 fi
6095 if test "$prctl_pr_set_timerslack" = "yes" ; then
6096   echo "CONFIG_PRCTL_PR_SET_TIMERSLACK=y" >> $config_host_mak
6097 fi
6098 if test "$epoll" = "yes" ; then
6099   echo "CONFIG_EPOLL=y" >> $config_host_mak
6100 fi
6101 if test "$epoll_create1" = "yes" ; then
6102   echo "CONFIG_EPOLL_CREATE1=y" >> $config_host_mak
6103 fi
6104 if test "$sendfile" = "yes" ; then
6105   echo "CONFIG_SENDFILE=y" >> $config_host_mak
6106 fi
6107 if test "$timerfd" = "yes" ; then
6108   echo "CONFIG_TIMERFD=y" >> $config_host_mak
6109 fi
6110 if test "$setns" = "yes" ; then
6111   echo "CONFIG_SETNS=y" >> $config_host_mak
6112 fi
6113 if test "$clock_adjtime" = "yes" ; then
6114   echo "CONFIG_CLOCK_ADJTIME=y" >> $config_host_mak
6115 fi
6116 if test "$syncfs" = "yes" ; then
6117   echo "CONFIG_SYNCFS=y" >> $config_host_mak
6118 fi
6119 if test "$inotify" = "yes" ; then
6120   echo "CONFIG_INOTIFY=y" >> $config_host_mak
6121 fi
6122 if test "$inotify1" = "yes" ; then
6123   echo "CONFIG_INOTIFY1=y" >> $config_host_mak
6124 fi
6125 if test "$sem_timedwait" = "yes" ; then
6126   echo "CONFIG_SEM_TIMEDWAIT=y" >> $config_host_mak
6127 fi
6128 if test "$strchrnul" = "yes" ; then
6129   echo "HAVE_STRCHRNUL=y" >> $config_host_mak
6130 fi
6131 if test "$st_atim" = "yes" ; then
6132   echo "HAVE_STRUCT_STAT_ST_ATIM=y" >> $config_host_mak
6133 fi
6134 if test "$byteswap_h" = "yes" ; then
6135   echo "CONFIG_BYTESWAP_H=y" >> $config_host_mak
6136 fi
6137 if test "$bswap_h" = "yes" ; then
6138   echo "CONFIG_MACHINE_BSWAP_H=y" >> $config_host_mak
6139 fi
6140 if test "$curl" = "yes" ; then
6141   echo "CONFIG_CURL=y" >> $config_host_mak
6142   echo "CURL_CFLAGS=$curl_cflags" >> $config_host_mak
6143   echo "CURL_LIBS=$curl_libs" >> $config_host_mak
6144 fi
6145 if test "$brlapi" = "yes" ; then
6146   echo "CONFIG_BRLAPI=y" >> $config_host_mak
6147   echo "BRLAPI_LIBS=$brlapi_libs" >> $config_host_mak
6148 fi
6149 if test "$gtk" = "yes" ; then
6150   echo "CONFIG_GTK=y" >> $config_host_mak
6151   echo "GTK_CFLAGS=$gtk_cflags" >> $config_host_mak
6152   echo "GTK_LIBS=$gtk_libs" >> $config_host_mak
6153   if test "$gtk_gl" = "yes" ; then
6154     echo "CONFIG_GTK_GL=y" >> $config_host_mak
6155   fi
6156 fi
6157 if test "$gio" = "yes" ; then
6158     echo "CONFIG_GIO=y" >> $config_host_mak
6159     echo "GIO_CFLAGS=$gio_cflags" >> $config_host_mak
6160     echo "GIO_LIBS=$gio_libs" >> $config_host_mak
6161     echo "GDBUS_CODEGEN=$gdbus_codegen" >> $config_host_mak
6162 fi
6163 echo "CONFIG_TLS_PRIORITY=\"$tls_priority\"" >> $config_host_mak
6164 if test "$gnutls" = "yes" ; then
6165   echo "CONFIG_GNUTLS=y" >> $config_host_mak
6166   echo "GNUTLS_CFLAGS=$gnutls_cflags" >> $config_host_mak
6167   echo "GNUTLS_LIBS=$gnutls_libs" >> $config_host_mak
6168 fi
6169 if test "$gcrypt" = "yes" ; then
6170   echo "CONFIG_GCRYPT=y" >> $config_host_mak
6171   if test "$gcrypt_hmac" = "yes" ; then
6172     echo "CONFIG_GCRYPT_HMAC=y" >> $config_host_mak
6173   fi
6174   echo "GCRYPT_CFLAGS=$gcrypt_cflags" >> $config_host_mak
6175   echo "GCRYPT_LIBS=$gcrypt_libs" >> $config_host_mak
6176 fi
6177 if test "$nettle" = "yes" ; then
6178   echo "CONFIG_NETTLE=y" >> $config_host_mak
6179   echo "CONFIG_NETTLE_VERSION_MAJOR=${nettle_version%%.*}" >> $config_host_mak
6180   echo "NETTLE_CFLAGS=$nettle_cflags" >> $config_host_mak
6181   echo "NETTLE_LIBS=$nettle_libs" >> $config_host_mak
6182 fi
6183 if test "$qemu_private_xts" = "yes" ; then
6184   echo "CONFIG_QEMU_PRIVATE_XTS=y" >> $config_host_mak
6185 fi
6186 if test "$tasn1" = "yes" ; then
6187   echo "CONFIG_TASN1=y" >> $config_host_mak
6188 fi
6189 if test "$auth_pam" = "yes" ; then
6190     echo "CONFIG_AUTH_PAM=y" >> $config_host_mak
6191 fi
6192 if test "$have_broken_size_max" = "yes" ; then
6193     echo "HAVE_BROKEN_SIZE_MAX=y" >> $config_host_mak
6194 fi
6195 if test "$have_openpty" = "yes" ; then
6196     echo "HAVE_OPENPTY=y" >> $config_host_mak
6197 fi
6198
6199 # Work around a system header bug with some kernel/XFS header
6200 # versions where they both try to define 'struct fsxattr':
6201 # xfs headers will not try to redefine structs from linux headers
6202 # if this macro is set.
6203 if test "$have_fsxattr" = "yes" ; then
6204     echo "HAVE_FSXATTR=y" >> $config_host_mak
6205 fi
6206 if test "$have_copy_file_range" = "yes" ; then
6207     echo "HAVE_COPY_FILE_RANGE=y" >> $config_host_mak
6208 fi
6209 if test "$vte" = "yes" ; then
6210   echo "CONFIG_VTE=y" >> $config_host_mak
6211   echo "VTE_CFLAGS=$vte_cflags" >> $config_host_mak
6212   echo "VTE_LIBS=$vte_libs" >> $config_host_mak
6213 fi
6214 if test "$virglrenderer" = "yes" ; then
6215   echo "CONFIG_VIRGL=y" >> $config_host_mak
6216   echo "VIRGL_CFLAGS=$virgl_cflags" >> $config_host_mak
6217   echo "VIRGL_LIBS=$virgl_libs" >> $config_host_mak
6218 fi
6219 if test "$xen" = "enabled" ; then
6220   echo "CONFIG_XEN_BACKEND=y" >> $config_host_mak
6221   echo "CONFIG_XEN_CTRL_INTERFACE_VERSION=$xen_ctrl_version" >> $config_host_mak
6222   echo "XEN_CFLAGS=$xen_cflags" >> $config_host_mak
6223   echo "XEN_LIBS=$xen_libs" >> $config_host_mak
6224 fi
6225 if test "$linux_aio" = "yes" ; then
6226   echo "CONFIG_LINUX_AIO=y" >> $config_host_mak
6227 fi
6228 if test "$linux_io_uring" = "yes" ; then
6229   echo "CONFIG_LINUX_IO_URING=y" >> $config_host_mak
6230   echo "LINUX_IO_URING_CFLAGS=$linux_io_uring_cflags" >> $config_host_mak
6231   echo "LINUX_IO_URING_LIBS=$linux_io_uring_libs" >> $config_host_mak
6232 fi
6233 if test "$attr" = "yes" ; then
6234   echo "CONFIG_ATTR=y" >> $config_host_mak
6235   echo "LIBATTR_LIBS=$libattr_libs" >> $config_host_mak
6236 fi
6237 if test "$libattr" = "yes" ; then
6238   echo "CONFIG_LIBATTR=y" >> $config_host_mak
6239 fi
6240 if test "$virtfs" = "yes" ; then
6241   echo "CONFIG_VIRTFS=y" >> $config_host_mak
6242 fi
6243 if test "$vhost_scsi" = "yes" ; then
6244   echo "CONFIG_VHOST_SCSI=y" >> $config_host_mak
6245 fi
6246 if test "$vhost_net" = "yes" ; then
6247   echo "CONFIG_VHOST_NET=y" >> $config_host_mak
6248 fi
6249 if test "$vhost_net_user" = "yes" ; then
6250   echo "CONFIG_VHOST_NET_USER=y" >> $config_host_mak
6251 fi
6252 if test "$vhost_net_vdpa" = "yes" ; then
6253   echo "CONFIG_VHOST_NET_VDPA=y" >> $config_host_mak
6254 fi
6255 if test "$vhost_crypto" = "yes" ; then
6256   echo "CONFIG_VHOST_CRYPTO=y" >> $config_host_mak
6257 fi
6258 if test "$vhost_vsock" = "yes" ; then
6259   echo "CONFIG_VHOST_VSOCK=y" >> $config_host_mak
6260   if test "$vhost_user" = "yes" ; then
6261     echo "CONFIG_VHOST_USER_VSOCK=y" >> $config_host_mak
6262   fi
6263 fi
6264 if test "$vhost_kernel" = "yes" ; then
6265   echo "CONFIG_VHOST_KERNEL=y" >> $config_host_mak
6266 fi
6267 if test "$vhost_user" = "yes" ; then
6268   echo "CONFIG_VHOST_USER=y" >> $config_host_mak
6269 fi
6270 if test "$vhost_vdpa" = "yes" ; then
6271   echo "CONFIG_VHOST_VDPA=y" >> $config_host_mak
6272 fi
6273 if test "$vhost_user_fs" = "yes" ; then
6274   echo "CONFIG_VHOST_USER_FS=y" >> $config_host_mak
6275 fi
6276 if test "$iovec" = "yes" ; then
6277   echo "CONFIG_IOVEC=y" >> $config_host_mak
6278 fi
6279 if test "$preadv" = "yes" ; then
6280   echo "CONFIG_PREADV=y" >> $config_host_mak
6281 fi
6282 if test "$membarrier" = "yes" ; then
6283   echo "CONFIG_MEMBARRIER=y" >> $config_host_mak
6284 fi
6285 if test "$signalfd" = "yes" ; then
6286   echo "CONFIG_SIGNALFD=y" >> $config_host_mak
6287 fi
6288 if test "$optreset" = "yes" ; then
6289   echo "HAVE_OPTRESET=y" >> $config_host_mak
6290 fi
6291 if test "$tcg" = "enabled"; then
6292   if test "$tcg_interpreter" = "yes" ; then
6293     echo "CONFIG_TCG_INTERPRETER=y" >> $config_host_mak
6294   fi
6295 fi
6296 if test "$fdatasync" = "yes" ; then
6297   echo "CONFIG_FDATASYNC=y" >> $config_host_mak
6298 fi
6299 if test "$madvise" = "yes" ; then
6300   echo "CONFIG_MADVISE=y" >> $config_host_mak
6301 fi
6302 if test "$posix_madvise" = "yes" ; then
6303   echo "CONFIG_POSIX_MADVISE=y" >> $config_host_mak
6304 fi
6305 if test "$posix_memalign" = "yes" ; then
6306   echo "CONFIG_POSIX_MEMALIGN=y" >> $config_host_mak
6307 fi
6308 if test "$spice" = "yes" ; then
6309   echo "CONFIG_SPICE=y" >> $config_host_mak
6310   echo "SPICE_CFLAGS=$spice_cflags" >> $config_host_mak
6311   echo "SPICE_LIBS=$spice_libs" >> $config_host_mak
6312 fi
6313
6314 if test "$smartcard" = "yes" ; then
6315   echo "CONFIG_SMARTCARD=y" >> $config_host_mak
6316   echo "SMARTCARD_CFLAGS=$libcacard_cflags" >> $config_host_mak
6317   echo "SMARTCARD_LIBS=$libcacard_libs" >> $config_host_mak
6318 fi
6319
6320 if test "$libusb" = "yes" ; then
6321   echo "CONFIG_USB_LIBUSB=y" >> $config_host_mak
6322   echo "LIBUSB_CFLAGS=$libusb_cflags" >> $config_host_mak
6323   echo "LIBUSB_LIBS=$libusb_libs" >> $config_host_mak
6324 fi
6325
6326 if test "$usb_redir" = "yes" ; then
6327   echo "CONFIG_USB_REDIR=y" >> $config_host_mak
6328   echo "USB_REDIR_CFLAGS=$usb_redir_cflags" >> $config_host_mak
6329   echo "USB_REDIR_LIBS=$usb_redir_libs" >> $config_host_mak
6330 fi
6331
6332 if test "$opengl" = "yes" ; then
6333   echo "CONFIG_OPENGL=y" >> $config_host_mak
6334   echo "OPENGL_CFLAGS=$opengl_cflags" >> $config_host_mak
6335   echo "OPENGL_LIBS=$opengl_libs" >> $config_host_mak
6336   if test "$opengl_dmabuf" = "yes" ; then
6337     echo "CONFIG_OPENGL_DMABUF=y" >> $config_host_mak
6338   fi
6339 fi
6340
6341 if test "$gbm" = "yes" ; then
6342     echo "CONFIG_GBM=y" >> $config_host_mak
6343     echo "GBM_LIBS=$gbm_libs" >> $config_host_mak
6344     echo "GBM_CFLAGS=$gbm_cflags" >> $config_host_mak
6345 fi
6346
6347
6348 if test "$avx2_opt" = "yes" ; then
6349   echo "CONFIG_AVX2_OPT=y" >> $config_host_mak
6350 fi
6351
6352 if test "$avx512f_opt" = "yes" ; then
6353   echo "CONFIG_AVX512F_OPT=y" >> $config_host_mak
6354 fi
6355
6356 if test "$lzo" = "yes" ; then
6357   echo "CONFIG_LZO=y" >> $config_host_mak
6358   echo "LZO_LIBS=$lzo_libs" >> $config_host_mak
6359 fi
6360
6361 if test "$snappy" = "yes" ; then
6362   echo "CONFIG_SNAPPY=y" >> $config_host_mak
6363   echo "SNAPPY_LIBS=$snappy_libs" >> $config_host_mak
6364 fi
6365
6366 if test "$bzip2" = "yes" ; then
6367   echo "CONFIG_BZIP2=y" >> $config_host_mak
6368   echo "BZIP2_LIBS=-lbz2" >> $config_host_mak
6369 fi
6370
6371 if test "$lzfse" = "yes" ; then
6372   echo "CONFIG_LZFSE=y" >> $config_host_mak
6373   echo "LZFSE_LIBS=-llzfse" >> $config_host_mak
6374 fi
6375
6376 if test "$zstd" = "yes" ; then
6377   echo "CONFIG_ZSTD=y" >> $config_host_mak
6378   echo "ZSTD_CFLAGS=$zstd_cflags" >> $config_host_mak
6379   echo "ZSTD_LIBS=$zstd_libs" >> $config_host_mak
6380 fi
6381
6382 if test "$libiscsi" = "yes" ; then
6383   echo "CONFIG_LIBISCSI=y" >> $config_host_mak
6384   echo "LIBISCSI_CFLAGS=$libiscsi_cflags" >> $config_host_mak
6385   echo "LIBISCSI_LIBS=$libiscsi_libs" >> $config_host_mak
6386 fi
6387
6388 if test "$libnfs" = "yes" ; then
6389   echo "CONFIG_LIBNFS=y" >> $config_host_mak
6390   echo "LIBNFS_LIBS=$libnfs_libs" >> $config_host_mak
6391 fi
6392
6393 if test "$seccomp" = "yes"; then
6394   echo "CONFIG_SECCOMP=y" >> $config_host_mak
6395   echo "SECCOMP_CFLAGS=$seccomp_cflags" >> $config_host_mak
6396   echo "SECCOMP_LIBS=$seccomp_libs" >> $config_host_mak
6397 fi
6398
6399 # XXX: suppress that
6400 if [ "$bsd" = "yes" ] ; then
6401   echo "CONFIG_BSD=y" >> $config_host_mak
6402 fi
6403
6404 if test "$qom_cast_debug" = "yes" ; then
6405   echo "CONFIG_QOM_CAST_DEBUG=y" >> $config_host_mak
6406 fi
6407 if test "$rbd" = "yes" ; then
6408   echo "CONFIG_RBD=y" >> $config_host_mak
6409   echo "RBD_LIBS=$rbd_libs" >> $config_host_mak
6410 fi
6411
6412 echo "CONFIG_COROUTINE_BACKEND=$coroutine" >> $config_host_mak
6413 if test "$coroutine_pool" = "yes" ; then
6414   echo "CONFIG_COROUTINE_POOL=1" >> $config_host_mak
6415 else
6416   echo "CONFIG_COROUTINE_POOL=0" >> $config_host_mak
6417 fi
6418
6419 if test "$debug_stack_usage" = "yes" ; then
6420   echo "CONFIG_DEBUG_STACK_USAGE=y" >> $config_host_mak
6421 fi
6422
6423 if test "$crypto_afalg" = "yes" ; then
6424   echo "CONFIG_AF_ALG=y" >> $config_host_mak
6425 fi
6426
6427 if test "$open_by_handle_at" = "yes" ; then
6428   echo "CONFIG_OPEN_BY_HANDLE=y" >> $config_host_mak
6429 fi
6430
6431 if test "$linux_magic_h" = "yes" ; then
6432   echo "CONFIG_LINUX_MAGIC_H=y" >> $config_host_mak
6433 fi
6434
6435 if test "$valgrind_h" = "yes" ; then
6436   echo "CONFIG_VALGRIND_H=y" >> $config_host_mak
6437 fi
6438
6439 if test "$have_asan_iface_fiber" = "yes" ; then
6440     echo "CONFIG_ASAN_IFACE_FIBER=y" >> $config_host_mak
6441 fi
6442
6443 if test "$have_tsan" = "yes" && test "$have_tsan_iface_fiber" = "yes" ; then
6444     echo "CONFIG_TSAN=y" >> $config_host_mak
6445 fi
6446
6447 if test "$has_environ" = "yes" ; then
6448   echo "CONFIG_HAS_ENVIRON=y" >> $config_host_mak
6449 fi
6450
6451 if test "$cpuid_h" = "yes" ; then
6452   echo "CONFIG_CPUID_H=y" >> $config_host_mak
6453 fi
6454
6455 if test "$int128" = "yes" ; then
6456   echo "CONFIG_INT128=y" >> $config_host_mak
6457 fi
6458
6459 if test "$atomic128" = "yes" ; then
6460   echo "CONFIG_ATOMIC128=y" >> $config_host_mak
6461 fi
6462
6463 if test "$cmpxchg128" = "yes" ; then
6464   echo "CONFIG_CMPXCHG128=y" >> $config_host_mak
6465 fi
6466
6467 if test "$atomic64" = "yes" ; then
6468   echo "CONFIG_ATOMIC64=y" >> $config_host_mak
6469 fi
6470
6471 if test "$attralias" = "yes" ; then
6472   echo "CONFIG_ATTRIBUTE_ALIAS=y" >> $config_host_mak
6473 fi
6474
6475 if test "$getauxval" = "yes" ; then
6476   echo "CONFIG_GETAUXVAL=y" >> $config_host_mak
6477 fi
6478
6479 if test "$glusterfs" = "yes" ; then
6480   echo "CONFIG_GLUSTERFS=y" >> $config_host_mak
6481   echo "GLUSTERFS_CFLAGS=$glusterfs_cflags" >> $config_host_mak
6482   echo "GLUSTERFS_LIBS=$glusterfs_libs" >> $config_host_mak
6483 fi
6484
6485 if test "$glusterfs_xlator_opt" = "yes" ; then
6486   echo "CONFIG_GLUSTERFS_XLATOR_OPT=y" >> $config_host_mak
6487 fi
6488
6489 if test "$glusterfs_discard" = "yes" ; then
6490   echo "CONFIG_GLUSTERFS_DISCARD=y" >> $config_host_mak
6491 fi
6492
6493 if test "$glusterfs_fallocate" = "yes" ; then
6494   echo "CONFIG_GLUSTERFS_FALLOCATE=y" >> $config_host_mak
6495 fi
6496
6497 if test "$glusterfs_zerofill" = "yes" ; then
6498   echo "CONFIG_GLUSTERFS_ZEROFILL=y" >> $config_host_mak
6499 fi
6500
6501 if test "$glusterfs_ftruncate_has_stat" = "yes" ; then
6502   echo "CONFIG_GLUSTERFS_FTRUNCATE_HAS_STAT=y" >> $config_host_mak
6503 fi
6504
6505 if test "$glusterfs_iocb_has_stat" = "yes" ; then
6506   echo "CONFIG_GLUSTERFS_IOCB_HAS_STAT=y" >> $config_host_mak
6507 fi
6508
6509 if test "$libssh" = "yes" ; then
6510   echo "CONFIG_LIBSSH=y" >> $config_host_mak
6511   echo "LIBSSH_CFLAGS=$libssh_cflags" >> $config_host_mak
6512   echo "LIBSSH_LIBS=$libssh_libs" >> $config_host_mak
6513 fi
6514
6515 if test "$live_block_migration" = "yes" ; then
6516   echo "CONFIG_LIVE_BLOCK_MIGRATION=y" >> $config_host_mak
6517 fi
6518
6519 if test "$tpm" = "yes"; then
6520   echo 'CONFIG_TPM=y' >> $config_host_mak
6521 fi
6522
6523 echo "TRACE_BACKENDS=$trace_backends" >> $config_host_mak
6524 if have_backend "nop"; then
6525   echo "CONFIG_TRACE_NOP=y" >> $config_host_mak
6526 fi
6527 if have_backend "simple"; then
6528   echo "CONFIG_TRACE_SIMPLE=y" >> $config_host_mak
6529   # Set the appropriate trace file.
6530   trace_file="\"$trace_file-\" FMT_pid"
6531 fi
6532 if have_backend "log"; then
6533   echo "CONFIG_TRACE_LOG=y" >> $config_host_mak
6534 fi
6535 if have_backend "ust"; then
6536   echo "CONFIG_TRACE_UST=y" >> $config_host_mak
6537   echo "LTTNG_UST_LIBS=$lttng_ust_libs" >> $config_host_mak
6538   echo "URCU_BP_LIBS=$urcu_bp_libs" >> $config_host_mak
6539 fi
6540 if have_backend "dtrace"; then
6541   echo "CONFIG_TRACE_DTRACE=y" >> $config_host_mak
6542   if test "$trace_backend_stap" = "yes" ; then
6543     echo "CONFIG_TRACE_SYSTEMTAP=y" >> $config_host_mak
6544   fi
6545 fi
6546 if have_backend "ftrace"; then
6547   if test "$linux" = "yes" ; then
6548     echo "CONFIG_TRACE_FTRACE=y" >> $config_host_mak
6549   else
6550     feature_not_found "ftrace(trace backend)" "ftrace requires Linux"
6551   fi
6552 fi
6553 if have_backend "syslog"; then
6554   if test "$posix_syslog" = "yes" ; then
6555     echo "CONFIG_TRACE_SYSLOG=y" >> $config_host_mak
6556   else
6557     feature_not_found "syslog(trace backend)" "syslog not available"
6558   fi
6559 fi
6560 echo "CONFIG_TRACE_FILE=$trace_file" >> $config_host_mak
6561
6562 if test "$rdma" = "yes" ; then
6563   echo "CONFIG_RDMA=y" >> $config_host_mak
6564   echo "RDMA_LIBS=$rdma_libs" >> $config_host_mak
6565 fi
6566
6567 if test "$pvrdma" = "yes" ; then
6568   echo "CONFIG_PVRDMA=y" >> $config_host_mak
6569 fi
6570
6571 if test "$have_rtnetlink" = "yes" ; then
6572   echo "CONFIG_RTNETLINK=y" >> $config_host_mak
6573 fi
6574
6575 if test "$libxml2" = "yes" ; then
6576   echo "CONFIG_LIBXML2=y" >> $config_host_mak
6577   echo "LIBXML2_CFLAGS=$libxml2_cflags" >> $config_host_mak
6578   echo "LIBXML2_LIBS=$libxml2_libs" >> $config_host_mak
6579 fi
6580
6581 if test "$replication" = "yes" ; then
6582   echo "CONFIG_REPLICATION=y" >> $config_host_mak
6583 fi
6584
6585 if test "$have_af_vsock" = "yes" ; then
6586   echo "CONFIG_AF_VSOCK=y" >> $config_host_mak
6587 fi
6588
6589 if test "$have_sysmacros" = "yes" ; then
6590   echo "CONFIG_SYSMACROS=y" >> $config_host_mak
6591 fi
6592
6593 if test "$have_static_assert" = "yes" ; then
6594   echo "CONFIG_STATIC_ASSERT=y" >> $config_host_mak
6595 fi
6596
6597 if test "$have_utmpx" = "yes" ; then
6598   echo "HAVE_UTMPX=y" >> $config_host_mak
6599 fi
6600 if test "$have_getrandom" = "yes" ; then
6601   echo "CONFIG_GETRANDOM=y" >> $config_host_mak
6602 fi
6603 if test "$ivshmem" = "yes" ; then
6604   echo "CONFIG_IVSHMEM=y" >> $config_host_mak
6605 fi
6606 if test "$debug_mutex" = "yes" ; then
6607   echo "CONFIG_DEBUG_MUTEX=y" >> $config_host_mak
6608 fi
6609
6610 # Hold two types of flag:
6611 #   CONFIG_THREAD_SETNAME_BYTHREAD  - we've got a way of setting the name on
6612 #                                     a thread we have a handle to
6613 #   CONFIG_PTHREAD_SETNAME_NP_W_TID - A way of doing it on a particular
6614 #                                     platform
6615 if test "$pthread_setname_np_w_tid" = "yes" ; then
6616   echo "CONFIG_THREAD_SETNAME_BYTHREAD=y" >> $config_host_mak
6617   echo "CONFIG_PTHREAD_SETNAME_NP_W_TID=y" >> $config_host_mak
6618 elif test "$pthread_setname_np_wo_tid" = "yes" ; then
6619   echo "CONFIG_THREAD_SETNAME_BYTHREAD=y" >> $config_host_mak
6620   echo "CONFIG_PTHREAD_SETNAME_NP_WO_TID=y" >> $config_host_mak
6621 fi
6622
6623 if test "$libpmem" = "yes" ; then
6624   echo "CONFIG_LIBPMEM=y" >> $config_host_mak
6625   echo "LIBPMEM_LIBS=$libpmem_libs" >> $config_host_mak
6626   echo "LIBPMEM_CFLAGS=$libpmem_cflags" >> $config_host_mak
6627 fi
6628
6629 if test "$libdaxctl" = "yes" ; then
6630   echo "CONFIG_LIBDAXCTL=y" >> $config_host_mak
6631   echo "LIBDAXCTL_LIBS=$libdaxctl_libs" >> $config_host_mak
6632 fi
6633
6634 if test "$bochs" = "yes" ; then
6635   echo "CONFIG_BOCHS=y" >> $config_host_mak
6636 fi
6637 if test "$cloop" = "yes" ; then
6638   echo "CONFIG_CLOOP=y" >> $config_host_mak
6639 fi
6640 if test "$dmg" = "yes" ; then
6641   echo "CONFIG_DMG=y" >> $config_host_mak
6642 fi
6643 if test "$qcow1" = "yes" ; then
6644   echo "CONFIG_QCOW1=y" >> $config_host_mak
6645 fi
6646 if test "$vdi" = "yes" ; then
6647   echo "CONFIG_VDI=y" >> $config_host_mak
6648 fi
6649 if test "$vvfat" = "yes" ; then
6650   echo "CONFIG_VVFAT=y" >> $config_host_mak
6651 fi
6652 if test "$qed" = "yes" ; then
6653   echo "CONFIG_QED=y" >> $config_host_mak
6654 fi
6655 if test "$parallels" = "yes" ; then
6656   echo "CONFIG_PARALLELS=y" >> $config_host_mak
6657 fi
6658 if test "$sheepdog" = "yes" ; then
6659   add_to deprecated_features "sheepdog"
6660   echo "CONFIG_SHEEPDOG=y" >> $config_host_mak
6661 fi
6662 if test "$have_mlockall" = "yes" ; then
6663   echo "HAVE_MLOCKALL=y" >> $config_host_mak
6664 fi
6665 if test "$fuzzing" = "yes" ; then
6666   # If LIB_FUZZING_ENGINE is set, assume we are running on OSS-Fuzz, and the
6667   # needed CFLAGS have already been provided
6668   if test -z "${LIB_FUZZING_ENGINE+xxx}" ; then
6669     QEMU_CFLAGS="$QEMU_CFLAGS -fsanitize=fuzzer-no-link"
6670     FUZZ_EXE_LDFLAGS="-fsanitize=fuzzer"
6671   else
6672     FUZZ_EXE_LDFLAGS="$LIB_FUZZING_ENGINE"
6673   fi
6674 fi
6675
6676 if test "$plugins" = "yes" ; then
6677     echo "CONFIG_PLUGIN=y" >> $config_host_mak
6678     # Copy the export object list to the build dir
6679     if test "$ld_dynamic_list" = "yes" ; then
6680         echo "CONFIG_HAS_LD_DYNAMIC_LIST=yes" >> $config_host_mak
6681         ld_symbols=qemu-plugins-ld.symbols
6682         cp "$source_path/plugins/qemu-plugins.symbols" $ld_symbols
6683     elif test "$ld_exported_symbols_list" = "yes" ; then
6684         echo "CONFIG_HAS_LD_EXPORTED_SYMBOLS_LIST=yes" >> $config_host_mak
6685         ld64_symbols=qemu-plugins-ld64.symbols
6686         echo "# Automatically generated by configure - do not modify" > $ld64_symbols
6687         grep 'qemu_' "$source_path/plugins/qemu-plugins.symbols" | sed 's/;//g' | \
6688             sed -E 's/^[[:space:]]*(.*)/_\1/' >> $ld64_symbols
6689     else
6690         error_exit \
6691             "If \$plugins=yes, either \$ld_dynamic_list or " \
6692             "\$ld_exported_symbols_list should have been set to 'yes'."
6693     fi
6694 fi
6695
6696 if test -n "$gdb_bin" ; then
6697     echo "HAVE_GDB_BIN=$gdb_bin" >> $config_host_mak
6698 fi
6699
6700 if test "$secret_keyring" = "yes" ; then
6701   echo "CONFIG_SECRET_KEYRING=y" >> $config_host_mak
6702 fi
6703
6704 echo "ROMS=$roms" >> $config_host_mak
6705 echo "MAKE=$make" >> $config_host_mak
6706 echo "PYTHON=$python" >> $config_host_mak
6707 echo "GENISOIMAGE=$genisoimage" >> $config_host_mak
6708 echo "MESON=$meson" >> $config_host_mak
6709 echo "NINJA=$ninja" >> $config_host_mak
6710 echo "CC=$cc" >> $config_host_mak
6711 if $iasl -h > /dev/null 2>&1; then
6712   echo "CONFIG_IASL=$iasl" >> $config_host_mak
6713 fi
6714 echo "CXX=$cxx" >> $config_host_mak
6715 echo "OBJCC=$objcc" >> $config_host_mak
6716 echo "AR=$ar" >> $config_host_mak
6717 echo "ARFLAGS=$ARFLAGS" >> $config_host_mak
6718 echo "AS=$as" >> $config_host_mak
6719 echo "CCAS=$ccas" >> $config_host_mak
6720 echo "CPP=$cpp" >> $config_host_mak
6721 echo "OBJCOPY=$objcopy" >> $config_host_mak
6722 echo "LD=$ld" >> $config_host_mak
6723 echo "RANLIB=$ranlib" >> $config_host_mak
6724 echo "NM=$nm" >> $config_host_mak
6725 echo "PKG_CONFIG=$pkg_config_exe" >> $config_host_mak
6726 echo "WINDRES=$windres" >> $config_host_mak
6727 echo "CFLAGS_NOPIE=$CFLAGS_NOPIE" >> $config_host_mak
6728 echo "QEMU_CFLAGS=$QEMU_CFLAGS" >> $config_host_mak
6729 echo "QEMU_CXXFLAGS=$QEMU_CXXFLAGS" >> $config_host_mak
6730 echo "GLIB_CFLAGS=$glib_cflags" >> $config_host_mak
6731 echo "GLIB_LIBS=$glib_libs" >> $config_host_mak
6732 echo "QEMU_LDFLAGS=$QEMU_LDFLAGS" >> $config_host_mak
6733 echo "LD_I386_EMULATION=$ld_i386_emulation" >> $config_host_mak
6734 echo "EXESUF=$EXESUF" >> $config_host_mak
6735 echo "HOST_DSOSUF=$HOST_DSOSUF" >> $config_host_mak
6736 echo "LIBS_QGA=$libs_qga" >> $config_host_mak
6737 echo "TASN1_LIBS=$tasn1_libs" >> $config_host_mak
6738 echo "TASN1_CFLAGS=$tasn1_cflags" >> $config_host_mak
6739 if test "$gcov" = "yes" ; then
6740   echo "CONFIG_GCOV=y" >> $config_host_mak
6741 fi
6742
6743 if test "$fuzzing" != "no"; then
6744     echo "CONFIG_FUZZ=y" >> $config_host_mak
6745 fi
6746 echo "FUZZ_EXE_LDFLAGS=$FUZZ_EXE_LDFLAGS" >> $config_host_mak
6747
6748 if test "$rng_none" = "yes"; then
6749   echo "CONFIG_RNG_NONE=y" >> $config_host_mak
6750 fi
6751
6752 # use included Linux headers
6753 if test "$linux" = "yes" ; then
6754   mkdir -p linux-headers
6755   case "$cpu" in
6756   i386|x86_64|x32)
6757     linux_arch=x86
6758     ;;
6759   ppc|ppc64|ppc64le)
6760     linux_arch=powerpc
6761     ;;
6762   s390x)
6763     linux_arch=s390
6764     ;;
6765   aarch64)
6766     linux_arch=arm64
6767     ;;
6768   mips64)
6769     linux_arch=mips
6770     ;;
6771   *)
6772     # For most CPUs the kernel architecture name and QEMU CPU name match.
6773     linux_arch="$cpu"
6774     ;;
6775   esac
6776     # For non-KVM architectures we will not have asm headers
6777     if [ -e "$source_path/linux-headers/asm-$linux_arch" ]; then
6778       symlink "$source_path/linux-headers/asm-$linux_arch" linux-headers/asm
6779     fi
6780 fi
6781
6782 for target in $target_list; do
6783     target_dir="$target"
6784     target_name=$(echo $target | cut -d '-' -f 1)
6785     mkdir -p $target_dir
6786     case $target in
6787         *-user) symlink "../qemu-$target_name" "$target_dir/qemu-$target_name" ;;
6788         *) symlink "../qemu-system-$target_name" "$target_dir/qemu-system-$target_name" ;;
6789     esac
6790 done
6791
6792 echo "CONFIG_QEMU_INTERP_PREFIX=$interp_prefix" | sed 's/%M/@0@/' >> $config_host_mak
6793 if test "$default_targets" = "yes"; then
6794   echo "CONFIG_DEFAULT_TARGETS=y" >> $config_host_mak
6795 fi
6796
6797 if test "$numa" = "yes"; then
6798   echo "CONFIG_NUMA=y" >> $config_host_mak
6799   echo "NUMA_LIBS=$numa_libs" >> $config_host_mak
6800 fi
6801
6802 if test "$ccache_cpp2" = "yes"; then
6803   echo "export CCACHE_CPP2=y" >> $config_host_mak
6804 fi
6805
6806 if test "$safe_stack" = "yes"; then
6807   echo "CONFIG_SAFESTACK=y" >> $config_host_mak
6808 fi
6809
6810 # If we're using a separate build tree, set it up now.
6811 # DIRS are directories which we simply mkdir in the build tree;
6812 # LINKS are things to symlink back into the source tree
6813 # (these can be both files and directories).
6814 # Caution: do not add files or directories here using wildcards. This
6815 # will result in problems later if a new file matching the wildcard is
6816 # added to the source tree -- nothing will cause configure to be rerun
6817 # so the build tree will be missing the link back to the new file, and
6818 # tests might fail. Prefer to keep the relevant files in their own
6819 # directory and symlink the directory instead.
6820 # UNLINK is used to remove symlinks from older development versions
6821 # that might get into the way when doing "git update" without doing
6822 # a "make distclean" in between.
6823 DIRS="tests tests/tcg tests/tcg/lm32 tests/qapi-schema tests/qtest/libqos"
6824 DIRS="$DIRS tests/qtest tests/qemu-iotests tests/vm tests/fp tests/qgraph"
6825 DIRS="$DIRS docs docs/interop fsdev scsi"
6826 DIRS="$DIRS pc-bios/optionrom pc-bios/s390-ccw"
6827 DIRS="$DIRS roms/seabios"
6828 DIRS="$DIRS contrib/plugins/"
6829 LINKS="Makefile"
6830 LINKS="$LINKS tests/tcg/lm32/Makefile"
6831 LINKS="$LINKS tests/tcg/Makefile.target"
6832 LINKS="$LINKS pc-bios/optionrom/Makefile"
6833 LINKS="$LINKS pc-bios/s390-ccw/Makefile"
6834 LINKS="$LINKS roms/seabios/Makefile"
6835 LINKS="$LINKS pc-bios/qemu-icon.bmp"
6836 LINKS="$LINKS .gdbinit scripts" # scripts needed by relative path in .gdbinit
6837 LINKS="$LINKS tests/acceptance tests/data"
6838 LINKS="$LINKS tests/qemu-iotests/check"
6839 LINKS="$LINKS python"
6840 LINKS="$LINKS contrib/plugins/Makefile "
6841 UNLINK="pc-bios/keymaps"
6842 for bios_file in \
6843     $source_path/pc-bios/*.bin \
6844     $source_path/pc-bios/*.elf \
6845     $source_path/pc-bios/*.lid \
6846     $source_path/pc-bios/*.rom \
6847     $source_path/pc-bios/*.dtb \
6848     $source_path/pc-bios/*.img \
6849     $source_path/pc-bios/openbios-* \
6850     $source_path/pc-bios/u-boot.* \
6851     $source_path/pc-bios/edk2-*.fd.bz2 \
6852     $source_path/pc-bios/palcode-*
6853 do
6854     LINKS="$LINKS pc-bios/$(basename $bios_file)"
6855 done
6856 mkdir -p $DIRS
6857 for f in $LINKS ; do
6858     if [ -e "$source_path/$f" ]; then
6859         symlink "$source_path/$f" "$f"
6860     fi
6861 done
6862 for f in $UNLINK ; do
6863     if [ -L "$f" ]; then
6864         rm -f "$f"
6865     fi
6866 done
6867
6868 (for i in $cross_cc_vars; do
6869   export $i
6870 done
6871 export target_list source_path use_containers
6872 $source_path/tests/tcg/configure.sh)
6873
6874 # temporary config to build submodules
6875 for rom in seabios; do
6876     config_mak=roms/$rom/config.mak
6877     echo "# Automatically generated by configure - do not modify" > $config_mak
6878     echo "SRC_PATH=$source_path/roms/$rom" >> $config_mak
6879     echo "AS=$as" >> $config_mak
6880     echo "CCAS=$ccas" >> $config_mak
6881     echo "CC=$cc" >> $config_mak
6882     echo "BCC=bcc" >> $config_mak
6883     echo "CPP=$cpp" >> $config_mak
6884     echo "OBJCOPY=objcopy" >> $config_mak
6885     echo "IASL=$iasl" >> $config_mak
6886     echo "LD=$ld" >> $config_mak
6887     echo "RANLIB=$ranlib" >> $config_mak
6888 done
6889
6890 # set up qemu-iotests in this build directory
6891 iotests_common_env="tests/qemu-iotests/common.env"
6892
6893 echo "# Automatically generated by configure - do not modify" > "$iotests_common_env"
6894 echo >> "$iotests_common_env"
6895 echo "export PYTHON='$python'" >> "$iotests_common_env"
6896
6897 if test "$skip_meson" = no; then
6898 cross="config-meson.cross.new"
6899 meson_quote() {
6900     echo "'$(echo $* | sed "s/ /','/g")'"
6901 }
6902
6903 echo "# Automatically generated by configure - do not modify" > $cross
6904 echo "[properties]" >> $cross
6905 test -z "$cxx" && echo "link_language = 'c'" >> $cross
6906 echo "[built-in options]" >> $cross
6907 echo "c_args = [${CFLAGS:+$(meson_quote $CFLAGS)}]" >> $cross
6908 echo "cpp_args = [${CXXFLAGS:+$(meson_quote $CXXFLAGS)}]" >> $cross
6909 echo "c_link_args = [${LDFLAGS:+$(meson_quote $LDFLAGS)}]" >> $cross
6910 echo "cpp_link_args = [${LDFLAGS:+$(meson_quote $LDFLAGS)}]" >> $cross
6911 echo "[binaries]" >> $cross
6912 echo "c = [$(meson_quote $cc)]" >> $cross
6913 test -n "$cxx" && echo "cpp = [$(meson_quote $cxx)]" >> $cross
6914 echo "ar = [$(meson_quote $ar)]" >> $cross
6915 echo "nm = [$(meson_quote $nm)]" >> $cross
6916 echo "pkgconfig = [$(meson_quote $pkg_config_exe)]" >> $cross
6917 echo "ranlib = [$(meson_quote $ranlib)]" >> $cross
6918 if has $sdl2_config; then
6919   echo "sdl2-config = [$(meson_quote $sdl2_config)]" >> $cross
6920 fi
6921 echo "strip = [$(meson_quote $strip)]" >> $cross
6922 echo "windres = [$(meson_quote $windres)]" >> $cross
6923 if test -n "$cross_prefix"; then
6924     cross_arg="--cross-file config-meson.cross"
6925     echo "[host_machine]" >> $cross
6926     if test "$mingw32" = "yes" ; then
6927         echo "system = 'windows'" >> $cross
6928     fi
6929     if test "$linux" = "yes" ; then
6930         echo "system = 'linux'" >> $cross
6931     fi
6932     case "$ARCH" in
6933         i386|x86_64)
6934             echo "cpu_family = 'x86'" >> $cross
6935             ;;
6936         ppc64le)
6937             echo "cpu_family = 'ppc64'" >> $cross
6938             ;;
6939         *)
6940             echo "cpu_family = '$ARCH'" >> $cross
6941             ;;
6942     esac
6943     echo "cpu = '$cpu'" >> $cross
6944     if test "$bigendian" = "yes" ; then
6945         echo "endian = 'big'" >> $cross
6946     else
6947         echo "endian = 'little'" >> $cross
6948     fi
6949 else
6950     cross_arg="--native-file config-meson.cross"
6951 fi
6952 mv $cross config-meson.cross
6953
6954 rm -rf meson-private meson-info meson-logs
6955 unset staticpic
6956 if ! version_ge "$($meson --version)" 0.56.0; then
6957   staticpic=$(if test "$pie" = yes; then echo true; else echo false; fi)
6958 fi
6959 NINJA=$ninja $meson setup \
6960         --prefix "$prefix" \
6961         --libdir "$libdir" \
6962         --libexecdir "$libexecdir" \
6963         --bindir "$bindir" \
6964         --includedir "$includedir" \
6965         --datadir "$datadir" \
6966         --mandir "$mandir" \
6967         --sysconfdir "$sysconfdir" \
6968         --localedir "$localedir" \
6969         --localstatedir "$local_statedir" \
6970         -Ddocdir="$docdir" \
6971         -Dqemu_firmwarepath="$firmwarepath" \
6972         -Dqemu_suffix="$qemu_suffix" \
6973         -Doptimization=$(if test "$debug" = yes; then echo 0; else echo 2; fi) \
6974         -Ddebug=$(if test "$debug_info" = yes; then echo true; else echo false; fi) \
6975         -Dwerror=$(if test "$werror" = yes; then echo true; else echo false; fi) \
6976         -Dstrip=$(if test "$strip_opt" = yes; then echo true; else echo false; fi) \
6977         -Db_pie=$(if test "$pie" = yes; then echo true; else echo false; fi) \
6978         ${staticpic:+-Db_staticpic=$staticpic} \
6979         -Db_coverage=$(if test "$gcov" = yes; then echo true; else echo false; fi) \
6980         -Db_lto=$lto -Dcfi=$cfi -Dcfi_debug=$cfi_debug \
6981         -Dmalloc=$malloc -Dmalloc_trim=$malloc_trim -Dsparse=$sparse \
6982         -Dkvm=$kvm -Dhax=$hax -Dwhpx=$whpx -Dhvf=$hvf \
6983         -Dxen=$xen -Dxen_pci_passthrough=$xen_pci_passthrough -Dtcg=$tcg \
6984         -Dcocoa=$cocoa -Dmpath=$mpath -Dsdl=$sdl -Dsdl_image=$sdl_image \
6985         -Dvnc=$vnc -Dvnc_sasl=$vnc_sasl -Dvnc_jpeg=$vnc_jpeg -Dvnc_png=$vnc_png \
6986         -Dgettext=$gettext -Dxkbcommon=$xkbcommon -Du2f=$u2f -Dvirtiofsd=$virtiofsd \
6987         -Dcapstone=$capstone -Dslirp=$slirp -Dfdt=$fdt \
6988         -Diconv=$iconv -Dcurses=$curses -Dlibudev=$libudev\
6989         -Ddocs=$docs -Dsphinx_build=$sphinx_build -Dinstall_blobs=$blobs \
6990         -Dvhost_user_blk_server=$vhost_user_blk_server \
6991         -Dfuse=$fuse -Dfuse_lseek=$fuse_lseek \
6992         $(if test "$default_features" = no; then echo "-Dauto_features=disabled"; fi) \
6993         $cross_arg \
6994         "$PWD" "$source_path"
6995
6996 if test "$?" -ne 0 ; then
6997     error_exit "meson setup failed"
6998 fi
6999 fi
7000
7001 if test -n "${deprecated_features}"; then
7002     echo "Warning, deprecated features enabled."
7003     echo "Please see docs/system/deprecated.rst"
7004     echo "  features: ${deprecated_features}"
7005 fi
7006
7007 # Save the configure command line for later reuse.
7008 cat <<EOD >config.status
7009 #!/bin/sh
7010 # Generated by configure.
7011 # Run this file to recreate the current configuration.
7012 # Compiler output produced by configure, useful for debugging
7013 # configure, is in config.log if it exists.
7014 EOD
7015
7016 preserve_env() {
7017     envname=$1
7018
7019     eval envval=\$$envname
7020
7021     if test -n "$envval"
7022     then
7023         echo "$envname='$envval'" >> config.status
7024         echo "export $envname" >> config.status
7025     else
7026         echo "unset $envname" >> config.status
7027     fi
7028 }
7029
7030 # Preserve various env variables that influence what
7031 # features/build target configure will detect
7032 preserve_env AR
7033 preserve_env AS
7034 preserve_env CC
7035 preserve_env CPP
7036 preserve_env CXX
7037 preserve_env INSTALL
7038 preserve_env LD
7039 preserve_env LD_LIBRARY_PATH
7040 preserve_env LIBTOOL
7041 preserve_env MAKE
7042 preserve_env NM
7043 preserve_env OBJCOPY
7044 preserve_env PATH
7045 preserve_env PKG_CONFIG
7046 preserve_env PKG_CONFIG_LIBDIR
7047 preserve_env PKG_CONFIG_PATH
7048 preserve_env PYTHON
7049 preserve_env SDL2_CONFIG
7050 preserve_env SMBD
7051 preserve_env STRIP
7052 preserve_env WINDRES
7053
7054 printf "exec" >>config.status
7055 for i in "$0" "$@"; do
7056   test "$i" = --skip-meson || printf " '%s'" "$i" >>config.status
7057 done
7058 echo ' "$@"' >>config.status
7059 chmod +x config.status
7060
7061 rm -r "$TMPDIR1"