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