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