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