configure

   1 #!/bin/sh
   2 #
   3 # Fio configure script. Heavily influenced by the manual qemu configure
   4 # script. Sad this is easier than autoconf and enemies.
   5 #
   6
   7 # set temporary file name
   8 if test ! -z "$TMPDIR" ; then
   9     TMPDIR1="${TMPDIR}"
  10 elif test ! -z "$TEMPDIR" ; then
  11     TMPDIR1="${TEMPDIR}"
  12 else
  13     TMPDIR1="/tmp"
  14 fi
  15
  16 TMPC="${TMPDIR1}/fio-conf-${RANDOM}-$$-${RANDOM}.c"
  17 TMPC2="${TMPDIR1}/fio-conf-${RANDOM}-$$-${RANDOM}-2.c"
  18 TMPO="${TMPDIR1}/fio-conf-${RANDOM}-$$-${RANDOM}.o"
  19 TMPE="${TMPDIR1}/fio-conf-${RANDOM}-$$-${RANDOM}.exe"
  20
  21 # NB: do not call "exit" in the trap handler; this is buggy with some shells;
  22 # see <1285349658-3122-1-git-send-email-loic.minier@linaro.org>
  23 trap "rm -f $TMPC $TMPC2 $TMPO $TMPE" EXIT INT QUIT TERM
  24
  25 rm -rf config.log
  26
  27 config_host_mak="config-host.mak"
  28 config_host_h="config-host.h"
  29
  30 rm -rf $config_host_mak
  31 rm -rf $config_host_h
  32
  33 fatal() {
  34   echo $@
  35   echo "Configure failed, check config.log and/or the above output"
  36   rm -rf $config_host_mak
  37   rm -rf $config_host_h
  38   exit 1
  39 }
  40
  41 # Print result for each configuration test
  42 print_config() {
  43   printf "%-30s%s\n" "$1" "$2"
  44 }
  45
  46 # Default CFLAGS
  47 CFLAGS="-D_GNU_SOURCE -include config-host.h"
  48 BUILD_CFLAGS=""
  49
  50 # Print a helpful header at the top of config.log
  51 echo "# FIO configure log $(date)" >> config.log
  52 printf "# Configured with:" >> config.log
  53 printf " '%s'" "$0" "$@" >> config.log
  54 echo >> config.log
  55 echo "#" >> config.log
  56
  57 # Print configure header at the top of $config_host_h
  58 echo "/*" > $config_host_h
  59 echo " * Automatically generated by configure - do not modify" >> $config_host_h
  60 printf " * Configured with:" >> $config_host_h
  61 printf " * '%s'" "$0" "$@" >> $config_host_h
  62 echo "" >> $config_host_h
  63 echo " */" >> $config_host_h
  64
  65 do_cc() {
  66     # Run the compiler, capturing its output to the log.
  67     echo $cc "$@" >> config.log
  68     $cc "$@" >> config.log 2>&1 || return $?
  69     # Test passed. If this is an --enable-werror build, rerun
  70     # the test with -Werror and bail out if it fails. This
  71     # makes warning-generating-errors in configure test code
  72     # obvious to developers.
  73     if test "$werror" != "yes"; then
  74         return 0
  75     fi
  76     # Don't bother rerunning the compile if we were already using -Werror
  77     case "$*" in
  78         *-Werror*)
  79            return 0
  80         ;;
  81     esac
  82     echo $cc -Werror "$@" >> config.log
  83     $cc -Werror "$@" >> config.log 2>&1 && return $?
  84     echo "ERROR: configure test passed without -Werror but failed with -Werror."
  85     echo "This is probably a bug in the configure script. The failing command"
  86     echo "will be at the bottom of config.log."
  87     fatal "You can run configure with --disable-werror to bypass this check."
  88 }
  89
  90 compile_object() {
  91   do_cc $CFLAGS -Werror-implicit-function-declaration -c -o $TMPO $TMPC
  92 }
  93
  94 compile_prog() {
  95   local_cflags="$1"
  96   local_ldflags="$2 $LIBS"
  97   echo "Compiling test case $3" >> config.log
  98   do_cc $CFLAGS -Werror-implicit-function-declaration $local_cflags -o $TMPE $TMPC $LDFLAGS $local_ldflags
  99 }
 100
 101 feature_not_found() {
 102   feature=$1
 103   packages=$2
 104
 105   echo "ERROR"
 106   echo "ERROR: User requested feature $feature"
 107   if test ! -z "$packages" ; then
 108     echo "ERROR: That feature needs $packages installed"
 109   fi
 110   echo "ERROR: configure was not able to find it"
 111   fatal "ERROR"
 112 }
 113
 114 has() {
 115   type "$1" >/dev/null 2>&1
 116 }
 117
 118 check_define() {
 119   cat > $TMPC <<EOF
 120 #if !defined($1)
 121 #error $1 not defined
 122 #endif
 123 int main(void)
 124 {
 125   return 0;
 126 }
 127 EOF
 128   compile_object
 129 }
 130
 131 output_sym() {
 132   echo "$1=y" >> $config_host_mak
 133   echo "#define $1" >> $config_host_h
 134 }
 135
 136 targetos=""
 137 cpu=""
 138
 139 # default options
 140 show_help="no"
 141 exit_val=0
 142 gfio_check="no"
 143 libhdfs="no"
 144 pmemblk="no"
 145 devdax="no"
 146 pmem="no"
 147 disable_lex=""
 148 disable_pmem="no"
 149 disable_native="no"
 150 march_set="no"
 151 libiscsi="no"
 152 libnbd="no"
 153 libaio_uring="no"
 154 prefix=/usr/local
 155
 156 # parse options
 157 for opt do
 158   optarg=`expr "x$opt" : 'x[^=]*=\(.*\)'`
 159   case "$opt" in
 160   --prefix=*) prefix="$optarg"
 161   ;;
 162   --cpu=*) cpu="$optarg"
 163   ;;
 164   #  esx is cross compiled and cannot be detect through simple uname calls
 165   --esx)
 166   esx="yes"
 167   ;;
 168   --cc=*) CC="$optarg"
 169   ;;
 170   --extra-cflags=*) CFLAGS="$CFLAGS $optarg"
 171   ;;
 172   --build-32bit-win) build_32bit_win="yes"
 173   ;;
 174   --target-win-ver=*) target_win_ver="$optarg"
 175   ;;
 176   --build-static) build_static="yes"
 177   ;;
 178   --enable-gfio) gfio_check="yes"
 179   ;;
 180   --disable-numa) disable_numa="yes"
 181   ;;
 182   --disable-rdma) disable_rdma="yes"
 183   ;;
 184   --disable-rados) disable_rados="yes"
 185   ;;
 186   --disable-rbd) disable_rbd="yes"
 187   ;;
 188   --disable-http) disable_http="yes"
 189   ;;
 190   --disable-gfapi) disable_gfapi="yes"
 191   ;;
 192   --enable-libhdfs) libhdfs="yes"
 193   ;;
 194   --disable-lex) disable_lex="yes"
 195   ;;
 196   --enable-lex) disable_lex="no"
 197   ;;
 198   --disable-shm) no_shm="yes"
 199   ;;
 200   --disable-optimizations) disable_opt="yes"
 201   ;;
 202   --disable-pmem) disable_pmem="yes"
 203   ;;
 204   --enable-cuda) enable_cuda="yes"
 205   ;;
 206   --disable-native) disable_native="yes"
 207   ;;
 208   --with-ime=*) ime_path="$optarg"
 209   ;;
 210   --enable-libiscsi) libiscsi="yes"
 211   ;;
 212   --enable-libnbd) libnbd="yes"
 213   ;;
 214   --disable-tcmalloc) disable_tcmalloc="yes"
 215   ;;
 216   --enable-libaio-uring) libaio_uring="yes"
 217   ;;
 218   --help)
 219     show_help="yes"
 220     ;;
 221   *)
 222   echo "Bad option $opt"
 223   show_help="yes"
 224   exit_val=1
 225   esac
 226 done
 227
 228 if test "$show_help" = "yes" ; then
 229   echo "--prefix=               Use this directory as installation prefix"
 230   echo "--cpu=                  Specify target CPU if auto-detect fails"
 231   echo "--cc=                   Specify compiler to use"
 232   echo "--extra-cflags=         Specify extra CFLAGS to pass to compiler"
 233   echo "--build-32bit-win       Enable 32-bit build on Windows"
 234   echo "--target-win-ver=       Minimum version of Windows to target (XP or 7)"
 235   echo "--build-static          Build a static fio"
 236   echo "--esx                   Configure build options for esx"
 237   echo "--enable-gfio           Enable building of gtk gfio"
 238   echo "--disable-numa          Disable libnuma even if found"
 239   echo "--disable-rdma          Disable RDMA support even if found"
 240   echo "--disable-rados         Disable Rados support even if found"
 241   echo "--disable-rbd           Disable Rados Block Device even if found"
 242   echo "--disable-http          Disable HTTP support even if found"
 243   echo "--disable-gfapi         Disable gfapi"
 244   echo "--enable-libhdfs        Enable hdfs support"
 245   echo "--disable-lex           Disable use of lex/yacc for math"
 246   echo "--disable-pmem          Disable pmem based engines even if found"
 247   echo "--enable-lex            Enable use of lex/yacc for math"
 248   echo "--disable-shm           Disable SHM support"
 249   echo "--disable-optimizations Don't enable compiler optimizations"
 250   echo "--enable-cuda           Enable GPUDirect RDMA support"
 251   echo "--disable-native        Don't build for native host"
 252   echo "--with-ime=             Install path for DDN's Infinite Memory Engine"
 253   echo "--enable-libiscsi       Enable iscsi support"
 254   echo "--enable-libnbd         Enable libnbd (NBD engine) support"
 255   echo "--disable-tcmalloc      Disable tcmalloc support"
 256   echo "--enable-libaio-uring   Enable libaio emulated over io_uring"
 257   exit $exit_val
 258 fi
 259
 260 cross_prefix=${cross_prefix-${CROSS_COMPILE}}
 261 # Preferred compiler (can be overriden later after we know the platform):
 262 #  ${CC} (if set)
 263 #  ${cross_prefix}gcc (if cross-prefix specified)
 264 #  gcc if available
 265 #  clang if available
 266 if test -z "${CC}${cross_prefix}"; then
 267   if has gcc; then
 268     cc=gcc
 269   elif has clang; then
 270     cc=clang
 271   fi
 272 else
 273   cc="${CC-${cross_prefix}gcc}"
 274 fi
 275
 276 if check_define __ANDROID__ ; then
 277   targetos="Android"
 278 elif check_define __linux__ ; then
 279   targetos="Linux"
 280 elif check_define __OpenBSD__ ; then
 281   targetos='OpenBSD'
 282 elif check_define __NetBSD__ ; then
 283   targetos='NetBSD'
 284 elif check_define __sun__ ; then
 285   targetos='SunOS'
 286   CFLAGS="$CFLAGS -D_REENTRANT"
 287 elif check_define _WIN32 ; then
 288   targetos='CYGWIN'
 289 else
 290   targetos=`uname -s`
 291 fi
 292
 293 echo "# Automatically generated by configure - do not modify" > $config_host_mak
 294 printf "# Configured with:" >> $config_host_mak
 295 printf " '%s'" "$0" "$@" >> $config_host_mak
 296 echo >> $config_host_mak
 297 echo "CONFIG_TARGET_OS=$targetos" >> $config_host_mak
 298
 299 if test "$no_shm" = "yes" ; then
 300   output_sym "CONFIG_NO_SHM"
 301 fi
 302
 303 if test "$disable_opt" = "yes" ; then
 304   output_sym "CONFIG_FIO_NO_OPT"
 305 fi
 306
 307 # Some host OSes need non-standard checks for which CPU to use.
 308 # Note that these checks are broken for cross-compilation: if you're
 309 # cross-compiling to one of these OSes then you'll need to specify
 310 # the correct CPU with the --cpu option.
 311 case $targetos in
 312 AIX|OpenBSD|NetBSD)
 313   # Unless explicitly enabled, turn off lex.
 314   # OpenBSD will hit syntax error when enabled.
 315   if test -z "$disable_lex" ; then
 316     disable_lex="yes"
 317   else
 318     force_no_lex_o="yes"
 319   fi
 320   ;;
 321 FreeBSD)
 322   CFLAGS="$CFLAGS -I/usr/local/include"
 323   LDFLAGS="$LDFLAGS -L/usr/local/lib"
 324   ;;
 325 Darwin)
 326   # on Leopard most of the system is 32-bit, so we have to ask the kernel if
 327   # we can run 64-bit userspace code.
 328   # If the user didn't specify a CPU explicitly and the kernel says this is
 329   # 64 bit hw, then assume x86_64. Otherwise fall through to the usual
 330   # detection code.
 331   if test -z "$cpu" && test "$(sysctl -n hw.optional.x86_64)" = "1"; then
 332     cpu="x86_64"
 333   fi
 334   # Error at compile time linking of weak/partial symbols if possible...
 335 cat > $TMPC <<EOF
 336 int main(void)
 337 {
 338   return 0;
 339 }
 340 EOF
 341   if compile_prog "" "-Wl,-no_weak_imports" "disable weak symbols"; then
 342     echo "Disabling weak symbols"
 343     LDFLAGS="$LDFLAGS -Wl,-no_weak_imports"
 344   fi
 345   ;;
 346 SunOS)
 347   # `uname -m` returns i86pc even on an x86_64 box, so default based on isainfo
 348   if test -z "$cpu" && test "$(isainfo -k)" = "amd64"; then
 349     cpu="x86_64"
 350   fi
 351   LIBS="-lnsl -lsocket"
 352   ;;
 353 CYGWIN*)
 354   # We still force some options, so keep this message here.
 355   echo "Forcing some known good options on Windows"
 356   if test -z "${CC}${cross_prefix}"; then
 357     if test ! -z "$build_32bit_win" && test "$build_32bit_win" = "yes"; then
 358       cc="i686-w64-mingw32-gcc"
 359     else
 360       cc="x86_64-w64-mingw32-gcc"
 361     fi
 362   fi
 363
 364   target_win_ver=$(echo "$target_win_ver" | tr '[:lower:]' '[:upper:]')
 365   if test -z "$target_win_ver"; then
 366     # Default Windows API target
 367     target_win_ver="7"
 368   fi
 369   if test "$target_win_ver" = "XP"; then
 370     output_sym "CONFIG_WINDOWS_XP"
 371   elif test "$target_win_ver" = "7"; then
 372     output_sym "CONFIG_WINDOWS_7"
 373     CFLAGS="$CFLAGS -D_WIN32_WINNT=0x0601"
 374   else
 375     fatal "Unknown target Windows version"
 376   fi
 377
 378   # We need this to be output_sym'd here because this is Windows specific.
 379   # The regular configure path never sets this config.
 380   output_sym "CONFIG_WINDOWSAIO"
 381   # We now take the regular configuration path without having exit 0 here.
 382   # Flags below are still necessary mostly for MinGW.
 383   build_static="yes"
 384   socklen_t="yes"
 385   rusage_thread="yes"
 386   fdatasync="yes"
 387   clock_gettime="yes" # clock_monotonic probe has dependency on this
 388   clock_monotonic="yes"
 389   gettimeofday="yes"
 390   sched_idle="yes"
 391   tcp_nodelay="yes"
 392   ipv6="yes"
 393   ;;
 394 esac
 395
 396 # Now we know the target platform we can have another guess at the preferred
 397 # compiler when it wasn't explictly set
 398 if test -z "${CC}${cross_prefix}"; then
 399   if test "$targetos" = "FreeBSD" || test "$targetos" = "Darwin"; then
 400     if has clang; then
 401       cc=clang
 402     fi
 403   fi
 404 fi
 405 if test -z "$cc"; then
 406     echo "configure: failed to find compiler"
 407     exit 1
 408 fi
 409
 410 if test ! -z "$cpu" ; then
 411   # command line argument
 412   :
 413 elif check_define __i386__ ; then
 414   cpu="i386"
 415 elif check_define __x86_64__ ; then
 416   cpu="x86_64"
 417 elif check_define __sparc__ ; then
 418   if check_define __arch64__ ; then
 419     cpu="sparc64"
 420   else
 421     cpu="sparc"
 422   fi
 423 elif check_define _ARCH_PPC ; then
 424   if check_define _ARCH_PPC64 ; then
 425     cpu="ppc64"
 426   else
 427     cpu="ppc"
 428   fi
 429 elif check_define __mips__ ; then
 430   cpu="mips"
 431 elif check_define __ia64__ ; then
 432   cpu="ia64"
 433 elif check_define __s390__ ; then
 434   if check_define __s390x__ ; then
 435     cpu="s390x"
 436   else
 437     cpu="s390"
 438   fi
 439 elif check_define __arm__ ; then
 440   cpu="arm"
 441 elif check_define __aarch64__ ; then
 442   cpu="aarch64"
 443 elif check_define __hppa__ ; then
 444   cpu="hppa"
 445 else
 446   cpu=`uname -m`
 447 fi
 448
 449 # Normalise host CPU name and set ARCH.
 450 case "$cpu" in
 451   ia64|ppc|ppc64|s390|s390x|sparc64)
 452     cpu="$cpu"
 453   ;;
 454   i386|i486|i586|i686|i86pc|BePC)
 455     cpu="x86"
 456   ;;
 457   x86_64|amd64)
 458     cpu="x86_64"
 459   ;;
 460   armv*b|armv*l|arm)
 461     cpu="arm"
 462   ;;
 463   aarch64)
 464     cpu="arm64"
 465   ;;
 466   hppa|parisc|parisc64)
 467     cpu="hppa"
 468   ;;
 469   mips*)
 470     cpu="mips"
 471   ;;
 472   sparc|sun4[cdmuv])
 473     cpu="sparc"
 474   ;;
 475   *)
 476   echo "Unknown CPU"
 477   ;;
 478 esac
 479
 480 ##########################################
 481 # check cross compile
 482
 483 if test "$cross_compile" != "yes" ; then
 484   cross_compile="no"
 485 fi
 486 cat > $TMPC <<EOF
 487 int main(void)
 488 {
 489   return 0;
 490 }
 491 EOF
 492 if compile_prog "" "" "cross"; then
 493   $TMPE 2>/dev/null || cross_compile="yes"
 494 else
 495   fatal "compile test failed"
 496 fi
 497
 498 ##########################################
 499 # check endianness
 500 if test "$bigendian" != "yes" ; then
 501   bigendian="no"
 502 fi
 503 if test "$cross_compile" = "no" ; then
 504   cat > $TMPC <<EOF
 505 #include <inttypes.h>
 506 int main(void)
 507 {
 508   volatile uint32_t i=0x01234567;
 509   return (*((uint8_t*)(&i))) == 0x67;
 510 }
 511 EOF
 512   if compile_prog "" "" "endian"; then
 513     $TMPE && bigendian="yes"
 514   fi
 515 else
 516   # If we're cross compiling, try our best to work it out and rely on the
 517   # run-time check to fail if we get it wrong.
 518   cat > $TMPC <<EOF
 519 #include <endian.h>
 520 int main(void)
 521 {
 522 #if __BYTE_ORDER != __BIG_ENDIAN
 523 # error "Unknown endianness"
 524 #endif
 525 }
 526 EOF
 527   compile_prog "" "" "endian" && bigendian="yes"
 528   check_define "__ARMEB__" && bigendian="yes"
 529   check_define "__MIPSEB__" && bigendian="yes"
 530 fi
 531
 532
 533 print_config "Operating system" "$targetos"
 534 print_config "CPU" "$cpu"
 535 print_config "Big endian" "$bigendian"
 536 if test ! -z "$target_win_ver"; then
 537   print_config "Target Windows version" "$target_win_ver"
 538 fi
 539 print_config "Compiler" "$cc"
 540 print_config "Cross compile" "$cross_compile"
 541 echo
 542
 543 ##########################################
 544 # See if we need to build a static build
 545 if test "$build_static" = "yes" ; then
 546   CFLAGS="$CFLAGS -ffunction-sections -fdata-sections"
 547   LDFLAGS="$LDFLAGS -static -Wl,--gc-sections"
 548 else
 549   build_static="no"
 550 fi
 551 print_config "Static build" "$build_static"
 552
 553 ##########################################
 554 # check for wordsize
 555 wordsize="0"
 556 cat > $TMPC <<EOF
 557 #include <limits.h>
 558 #define BUILD_BUG_ON(condition) ((void)sizeof(char[1 - 2*!!(condition)]))
 559 int main(void)
 560 {
 561   BUILD_BUG_ON(sizeof(long)*CHAR_BIT != WORDSIZE);
 562   return 0;
 563 }
 564 EOF
 565 if compile_prog "-DWORDSIZE=32" "" "wordsize"; then
 566   wordsize="32"
 567 elif compile_prog "-DWORDSIZE=64" "" "wordsize"; then
 568   wordsize="64"
 569 else
 570   fatal "Unknown wordsize"
 571 fi
 572 print_config "Wordsize" "$wordsize"
 573
 574 ##########################################
 575 # zlib probe
 576 if test "$zlib" != "yes" ; then
 577   zlib="no"
 578 fi
 579 cat > $TMPC <<EOF
 580 #include <zlib.h>
 581 int main(void)
 582 {
 583   z_stream stream;
 584   if (inflateInit(&stream) != Z_OK)
 585     return 1;
 586   return 0;
 587 }
 588 EOF
 589 if compile_prog "" "-lz" "zlib" ; then
 590   zlib=yes
 591   LIBS="-lz $LIBS"
 592 fi
 593 print_config "zlib" "$zlib"
 594
 595 ##########################################
 596 # linux-aio probe
 597 if test "$libaio" != "yes" ; then
 598   libaio="no"
 599 fi
 600 if test "$esx" != "yes" ; then
 601   cat > $TMPC <<EOF
 602 #include <libaio.h>
 603 #include <stddef.h>
 604 int main(void)
 605 {
 606   io_setup(0, NULL);
 607   return 0;
 608 }
 609 EOF
 610   if test "$libaio_uring" = "yes" && compile_prog "" "-luring" "libaio io_uring" ; then
 611     libaio=yes
 612     LIBS="-luring $LIBS"
 613   elif compile_prog "" "-laio" "libaio" ; then
 614     libaio=yes
 615     libaio_uring=no
 616     LIBS="-laio $LIBS"
 617   else
 618     if test "$libaio" = "yes" ; then
 619       feature_not_found "linux AIO" "libaio-dev or libaio-devel"
 620     fi
 621     libaio=no
 622     libaio_uring=no
 623   fi
 624 fi
 625 print_config "Linux AIO support" "$libaio"
 626 print_config "Linux AIO over io_uring" "$libaio_uring"
 627
 628 ##########################################
 629 # posix aio probe
 630 if test "$posix_aio" != "yes" ; then
 631   posix_aio="no"
 632 fi
 633 if test "$posix_aio_lrt" != "yes" ; then
 634   posix_aio_lrt="no"
 635 fi
 636 cat > $TMPC <<EOF
 637 #include <aio.h>
 638 int main(void)
 639 {
 640   struct aiocb cb;
 641   aio_read(&cb);
 642   return 0;
 643 }
 644 EOF
 645 if compile_prog "" "" "posixaio" ; then
 646   posix_aio="yes"
 647 elif compile_prog "" "-lrt" "posixaio -lrt"; then
 648   posix_aio="yes"
 649   posix_aio_lrt="yes"
 650   LIBS="-lrt $LIBS"
 651 fi
 652 print_config "POSIX AIO support" "$posix_aio"
 653 print_config "POSIX AIO support needs -lrt" "$posix_aio_lrt"
 654
 655 ##########################################
 656 # posix aio fsync probe
 657 if test "$posix_aio_fsync" != "yes" ; then
 658   posix_aio_fsync="no"
 659 fi
 660 if test "$posix_aio" = "yes" ; then
 661   cat > $TMPC <<EOF
 662 #include <fcntl.h>
 663 #include <aio.h>
 664 int main(void)
 665 {
 666   struct aiocb cb;
 667   return aio_fsync(O_SYNC, &cb);
 668   return 0;
 669 }
 670 EOF
 671   if compile_prog "" "$LIBS" "posix_aio_fsync" ; then
 672     posix_aio_fsync=yes
 673   fi
 674 fi
 675 print_config "POSIX AIO fsync" "$posix_aio_fsync"
 676
 677 ##########################################
 678 # POSIX pshared attribute probe
 679 if test "$posix_pshared" != "yes" ; then
 680   posix_pshared="no"
 681 fi
 682 cat > $TMPC <<EOF
 683 #include <unistd.h>
 684 int main(void)
 685 {
 686 #if defined(_POSIX_THREAD_PROCESS_SHARED) && ((_POSIX_THREAD_PROCESS_SHARED + 0) > 0)
 687 # if defined(__CYGWIN__)
 688 #  error "_POSIX_THREAD_PROCESS_SHARED is buggy on Cygwin"
 689 # elif defined(__APPLE__)
 690 #  include <AvailabilityMacros.h>
 691 #  include <TargetConditionals.h>
 692 #  if TARGET_OS_MAC && MAC_OS_X_VERSION_MIN_REQUIRED < 1070
 693 #   error "_POSIX_THREAD_PROCESS_SHARED is buggy/unsupported prior to OSX 10.7"
 694 #  endif
 695 # endif
 696 #else
 697 # error "_POSIX_THREAD_PROCESS_SHARED is unsupported"
 698 #endif
 699   return 0;
 700 }
 701 EOF
 702 if compile_prog "" "$LIBS" "posix_pshared" ; then
 703   posix_pshared=yes
 704 fi
 705 print_config "POSIX pshared support" "$posix_pshared"
 706
 707 ##########################################
 708 # POSIX pthread_condattr_setclock() probe
 709 if test "$pthread_condattr_setclock" != "yes" ; then
 710   pthread_condattr_setclock="no"
 711 fi
 712 cat > $TMPC <<EOF
 713 #include <pthread.h>
 714 int main(void)
 715 {
 716   pthread_condattr_t condattr;
 717   pthread_condattr_setclock(&condattr, CLOCK_MONOTONIC);
 718   return 0;
 719 }
 720 EOF
 721 if compile_prog "" "$LIBS" "pthread_condattr_setclock" ; then
 722   pthread_condattr_setclock=yes
 723 fi
 724 print_config "pthread_condattr_setclock() support" "$pthread_condattr_setclock"
 725
 726 ##########################################
 727 # solaris aio probe
 728 if test "$solaris_aio" != "yes" ; then
 729   solaris_aio="no"
 730 fi
 731 cat > $TMPC <<EOF
 732 #include <sys/types.h>
 733 #include <sys/asynch.h>
 734 #include <unistd.h>
 735 int main(void)
 736 {
 737   aio_result_t res;
 738   return aioread(0, NULL, 0, 0, SEEK_SET, &res);
 739   return 0;
 740 }
 741 EOF
 742 if compile_prog "" "-laio" "solarisaio" ; then
 743   solaris_aio=yes
 744   LIBS="-laio $LIBS"
 745 fi
 746 print_config "Solaris AIO support" "$solaris_aio"
 747
 748 ##########################################
 749 # __sync_fetch_and_add test
 750 if test "$sfaa" != "yes" ; then
 751   sfaa="no"
 752 fi
 753 cat > $TMPC << EOF
 754 #include <inttypes.h>
 755 static int sfaa(uint64_t *ptr)
 756 {
 757   return __sync_fetch_and_add(ptr, 0);
 758 }
 759
 760 int main(int argc, char **argv)
 761 {
 762   uint64_t val = 42;
 763   sfaa(&val);
 764   return val;
 765 }
 766 EOF
 767 if compile_prog "" "" "__sync_fetch_and_add()" ; then
 768     sfaa="yes"
 769 fi
 770 print_config "__sync_fetch_and_add" "$sfaa"
 771
 772 ##########################################
 773 # __sync_synchronize() test
 774 if test "$sync_sync" != "yes" ; then
 775   sync_sync="no"
 776 fi
 777 cat > $TMPC << EOF
 778 #include <inttypes.h>
 779
 780 int main(int argc, char **argv)
 781 {
 782   __sync_synchronize();
 783   return 0;
 784 }
 785 EOF
 786 if compile_prog "" "" "__sync_synchronize()" ; then
 787     sync_sync="yes"
 788 fi
 789 print_config "__sync_synchronize" "$sync_sync"
 790
 791 ##########################################
 792 # __sync_val_compare_and_swap() test
 793 if test "$cmp_swap" != "yes" ; then
 794   cmp_swap="no"
 795 fi
 796 cat > $TMPC << EOF
 797 #include <inttypes.h>
 798
 799 int main(int argc, char **argv)
 800 {
 801   int x = 0;
 802   return __sync_val_compare_and_swap(&x, 1, 2);
 803 }
 804 EOF
 805 if compile_prog "" "" "__sync_val_compare_and_swap()" ; then
 806     cmp_swap="yes"
 807 fi
 808 print_config "__sync_val_compare_and_swap" "$cmp_swap"
 809
 810 ##########################################
 811 # libverbs probe
 812 if test "$libverbs" != "yes" ; then
 813   libverbs="no"
 814 fi
 815 cat > $TMPC << EOF
 816 #include <infiniband/verbs.h>
 817 int main(int argc, char **argv)
 818 {
 819   struct ibv_pd *pd = ibv_alloc_pd(NULL);
 820   return 0;
 821 }
 822 EOF
 823 if test "$disable_rdma" != "yes" && compile_prog "" "-libverbs" "libverbs" ; then
 824     libverbs="yes"
 825     LIBS="-libverbs $LIBS"
 826 fi
 827 print_config "libverbs" "$libverbs"
 828
 829 ##########################################
 830 # rdmacm probe
 831 if test "$rdmacm" != "yes" ; then
 832   rdmacm="no"
 833 fi
 834 cat > $TMPC << EOF
 835 #include <stdio.h>
 836 #include <rdma/rdma_cma.h>
 837 int main(int argc, char **argv)
 838 {
 839   rdma_destroy_qp(NULL);
 840   return 0;
 841 }
 842 EOF
 843 if test "$disable_rdma" != "yes" && compile_prog "" "-lrdmacm" "rdma"; then
 844     rdmacm="yes"
 845     LIBS="-lrdmacm $LIBS"
 846 fi
 847 print_config "rdmacm" "$rdmacm"
 848
 849 ##########################################
 850 # asprintf() and vasprintf() probes
 851 if test "$have_asprintf" != "yes" ; then
 852   have_asprintf="no"
 853 fi
 854 cat > $TMPC << EOF
 855 #include <stdio.h>
 856
 857 int main(int argc, char **argv)
 858 {
 859   return asprintf(NULL, "%s", "str") == 0;
 860 }
 861 EOF
 862 if compile_prog "" "" "have_asprintf"; then
 863     have_asprintf="yes"
 864 fi
 865 print_config "asprintf()" "$have_asprintf"
 866
 867 if test "$have_vasprintf" != "yes" ; then
 868   have_vasprintf="no"
 869 fi
 870 cat > $TMPC << EOF
 871 #include <stdio.h>
 872
 873 int main(int argc, char **argv)
 874 {
 875   return vasprintf(NULL, "%s", NULL) == 0;
 876 }
 877 EOF
 878 if compile_prog "" "" "have_vasprintf"; then
 879     have_vasprintf="yes"
 880 fi
 881 print_config "vasprintf()" "$have_vasprintf"
 882
 883 ##########################################
 884 # Linux fallocate probe
 885 if test "$linux_fallocate" != "yes" ; then
 886   linux_fallocate="no"
 887 fi
 888 cat > $TMPC << EOF
 889 #include <stdio.h>
 890 #include <fcntl.h>
 891 #include <linux/falloc.h>
 892 int main(int argc, char **argv)
 893 {
 894   int r = fallocate(0, FALLOC_FL_KEEP_SIZE, 0, 1024);
 895   return r;
 896 }
 897 EOF
 898 if compile_prog "" "" "linux_fallocate"; then
 899     linux_fallocate="yes"
 900 fi
 901 print_config "Linux fallocate" "$linux_fallocate"
 902
 903 ##########################################
 904 # POSIX fadvise probe
 905 if test "$posix_fadvise" != "yes" ; then
 906   posix_fadvise="no"
 907 fi
 908 cat > $TMPC << EOF
 909 #include <stdio.h>
 910 #include <fcntl.h>
 911 int main(int argc, char **argv)
 912 {
 913   int r = posix_fadvise(0, 0, 0, POSIX_FADV_NORMAL);
 914   return r;
 915 }
 916 EOF
 917 if compile_prog "" "" "posix_fadvise"; then
 918     posix_fadvise="yes"
 919 fi
 920 print_config "POSIX fadvise" "$posix_fadvise"
 921
 922 ##########################################
 923 # POSIX fallocate probe
 924 if test "$posix_fallocate" != "yes" ; then
 925   posix_fallocate="no"
 926 fi
 927 cat > $TMPC << EOF
 928 #include <stdio.h>
 929 #include <fcntl.h>
 930 int main(int argc, char **argv)
 931 {
 932   int r = posix_fallocate(0, 0, 1024);
 933   return r;
 934 }
 935 EOF
 936 if compile_prog "" "" "posix_fallocate"; then
 937     posix_fallocate="yes"
 938 fi
 939 print_config "POSIX fallocate" "$posix_fallocate"
 940
 941 ##########################################
 942 # sched_set/getaffinity 2 or 3 argument test
 943 if test "$linux_2arg_affinity" != "yes" ; then
 944   linux_2arg_affinity="no"
 945 fi
 946 if test "$linux_3arg_affinity" != "yes" ; then
 947   linux_3arg_affinity="no"
 948 fi
 949 cat > $TMPC << EOF
 950 #include <sched.h>
 951 int main(int argc, char **argv)
 952 {
 953   cpu_set_t mask;
 954   return sched_setaffinity(0, sizeof(mask), &mask);
 955 }
 956 EOF
 957 if compile_prog "" "" "sched_setaffinity(,,)"; then
 958   linux_3arg_affinity="yes"
 959 else
 960   cat > $TMPC << EOF
 961 #include <sched.h>
 962 int main(int argc, char **argv)
 963 {
 964   cpu_set_t mask;
 965   return sched_setaffinity(0, &mask);
 966 }
 967 EOF
 968   if compile_prog "" "" "sched_setaffinity(,)"; then
 969     linux_2arg_affinity="yes"
 970   fi
 971 fi
 972 print_config "sched_setaffinity(3 arg)" "$linux_3arg_affinity"
 973 print_config "sched_setaffinity(2 arg)" "$linux_2arg_affinity"
 974
 975 ##########################################
 976 # clock_gettime probe
 977 if test "$clock_gettime" != "yes" ; then
 978   clock_gettime="no"
 979 fi
 980 cat > $TMPC << EOF
 981 #include <stdio.h>
 982 #include <time.h>
 983 int main(int argc, char **argv)
 984 {
 985   return clock_gettime(0, NULL);
 986 }
 987 EOF
 988 if compile_prog "" "" "clock_gettime"; then
 989     clock_gettime="yes"
 990 elif compile_prog "" "-lrt" "clock_gettime"; then
 991     clock_gettime="yes"
 992     LIBS="-lrt $LIBS"
 993 fi
 994 print_config "clock_gettime" "$clock_gettime"
 995
 996 ##########################################
 997 # CLOCK_MONOTONIC probe
 998 if test "$clock_monotonic" != "yes" ; then
 999   clock_monotonic="no"
1000 fi
1001 if test "$clock_gettime" = "yes" ; then
1002   cat > $TMPC << EOF
1003 #include <stdio.h>
1004 #include <time.h>
1005 int main(int argc, char **argv)
1006 {
1007   return clock_gettime(CLOCK_MONOTONIC, NULL);
1008 }
1009 EOF
1010   if compile_prog "" "$LIBS" "clock monotonic"; then
1011       clock_monotonic="yes"
1012   fi
1013 fi
1014 print_config "CLOCK_MONOTONIC" "$clock_monotonic"
1015
1016 ##########################################
1017 # CLOCK_MONOTONIC_RAW probe
1018 if test "$clock_monotonic_raw" != "yes" ; then
1019   clock_monotonic_raw="no"
1020 fi
1021 if test "$clock_gettime" = "yes" ; then
1022   cat > $TMPC << EOF
1023 #include <stdio.h>
1024 #include <time.h>
1025 int main(int argc, char **argv)
1026 {
1027   return clock_gettime(CLOCK_MONOTONIC_RAW, NULL);
1028 }
1029 EOF
1030   if compile_prog "" "$LIBS" "clock monotonic"; then
1031       clock_monotonic_raw="yes"
1032   fi
1033 fi
1034 print_config "CLOCK_MONOTONIC_RAW" "$clock_monotonic_raw"
1035
1036 ##########################################
1037 # CLOCK_MONOTONIC_PRECISE probe
1038 if test "$clock_monotonic_precise" != "yes" ; then
1039   clock_monotonic_precise="no"
1040 fi
1041 if test "$clock_gettime" = "yes" ; then
1042   cat > $TMPC << EOF
1043 #include <stdio.h>
1044 #include <time.h>
1045 int main(int argc, char **argv)
1046 {
1047   return clock_gettime(CLOCK_MONOTONIC_PRECISE, NULL);
1048 }
1049 EOF
1050   if compile_prog "" "$LIBS" "clock monotonic precise"; then
1051       clock_monotonic_precise="yes"
1052   fi
1053 fi
1054 print_config "CLOCK_MONOTONIC_PRECISE" "$clock_monotonic_precise"
1055
1056 ##########################################
1057 # clockid_t probe
1058 if test "$clockid_t" != "yes" ; then
1059   clockid_t="no"
1060 fi
1061 cat > $TMPC << EOF
1062 #include <time.h>
1063 #include <string.h>
1064 int main(int argc, char **argv)
1065 {
1066   volatile clockid_t cid;
1067   memset((void*)&cid, 0, sizeof(cid));
1068   return 0;
1069 }
1070 EOF
1071 if compile_prog "" "$LIBS" "clockid_t"; then
1072   clockid_t="yes"
1073 fi
1074 print_config "clockid_t" "$clockid_t"
1075
1076 ##########################################
1077 # gettimeofday() probe
1078 if test "$gettimeofday" != "yes" ; then
1079   gettimeofday="no"
1080 fi
1081 cat > $TMPC << EOF
1082 #include <sys/time.h>
1083 #include <stdio.h>
1084 int main(int argc, char **argv)
1085 {
1086   struct timeval tv;
1087   return gettimeofday(&tv, NULL);
1088 }
1089 EOF
1090 if compile_prog "" "" "gettimeofday"; then
1091     gettimeofday="yes"
1092 fi
1093 print_config "gettimeofday" "$gettimeofday"
1094
1095 ##########################################
1096 # fdatasync() probe
1097 if test "$fdatasync" != "yes" ; then
1098   fdatasync="no"
1099 fi
1100 cat > $TMPC << EOF
1101 #include <stdio.h>
1102 #include <unistd.h>
1103 int main(int argc, char **argv)
1104 {
1105   return fdatasync(0);
1106 }
1107 EOF
1108 if compile_prog "" "" "fdatasync"; then
1109   fdatasync="yes"
1110 fi
1111 print_config "fdatasync" "$fdatasync"
1112
1113 ##########################################
1114 # sync_file_range() probe
1115 if test "$sync_file_range" != "yes" ; then
1116   sync_file_range="no"
1117 fi
1118 cat > $TMPC << EOF
1119 #include <stdio.h>
1120 #include <unistd.h>
1121 #include <fcntl.h>
1122 #include <linux/fs.h>
1123 int main(int argc, char **argv)
1124 {
1125   unsigned int flags = SYNC_FILE_RANGE_WAIT_BEFORE | SYNC_FILE_RANGE_WRITE |
1126                         SYNC_FILE_RANGE_WAIT_AFTER;
1127   return sync_file_range(0, 0, 0, flags);
1128 }
1129 EOF
1130 if compile_prog "" "" "sync_file_range"; then
1131   sync_file_range="yes"
1132 fi
1133 print_config "sync_file_range" "$sync_file_range"
1134
1135 ##########################################
1136 # ext4 move extent probe
1137 if test "$ext4_me" != "yes" ; then
1138   ext4_me="no"
1139 fi
1140 cat > $TMPC << EOF
1141 #include <fcntl.h>
1142 #include <sys/ioctl.h>
1143 int main(int argc, char **argv)
1144 {
1145   struct move_extent me;
1146   return ioctl(0, EXT4_IOC_MOVE_EXT, &me);
1147 }
1148 EOF
1149 if compile_prog "" "" "ext4 move extent" ; then
1150   ext4_me="yes"
1151 elif test $targetos = "Linux" ; then
1152   # On Linux, just default to it on and let it error at runtime if we really
1153   # don't have it. None of my updated systems have it defined, but it does
1154   # work. Takes a while to bubble back.
1155   ext4_me="yes"
1156 fi
1157 print_config "EXT4 move extent" "$ext4_me"
1158
1159 ##########################################
1160 # splice probe
1161 if test "$linux_splice" != "yes" ; then
1162   linux_splice="no"
1163 fi
1164 cat > $TMPC << EOF
1165 #include <stdio.h>
1166 #include <fcntl.h>
1167 int main(int argc, char **argv)
1168 {
1169   return splice(0, NULL, 0, NULL, 0, SPLICE_F_NONBLOCK);
1170 }
1171 EOF
1172 if compile_prog "" "" "linux splice"; then
1173   linux_splice="yes"
1174 fi
1175 print_config "Linux splice(2)" "$linux_splice"
1176
1177 ##########################################
1178 # GUASI probe
1179 if test "$guasi" != "yes" ; then
1180   guasi="no"
1181 fi
1182 cat > $TMPC << EOF
1183 #include <guasi.h>
1184 #include <guasi_syscalls.h>
1185 int main(int argc, char **argv)
1186 {
1187   guasi_t ctx = guasi_create(0, 0, 0);
1188   return 0;
1189 }
1190 EOF
1191 if compile_prog "" "" "guasi"; then
1192   guasi="yes"
1193 fi
1194 print_config "GUASI" "$guasi"
1195
1196 ##########################################
1197 # libnuma probe
1198 if test "$libnuma" != "yes" ; then
1199   libnuma="no"
1200 fi
1201 cat > $TMPC << EOF
1202 #include <numa.h>
1203 int main(int argc, char **argv)
1204 {
1205   return numa_available();
1206 }
1207 EOF
1208 if test "$disable_numa" != "yes"  && compile_prog "" "-lnuma" "libnuma"; then
1209   libnuma="yes"
1210   LIBS="-lnuma $LIBS"
1211 fi
1212 print_config "libnuma" "$libnuma"
1213
1214 ##########################################
1215 # libnuma 2.x version API, initialize with "no" only if $libnuma is set to "yes"
1216 if test "$libnuma" = "yes" ; then
1217 libnuma_v2="no"
1218 cat > $TMPC << EOF
1219 #include <numa.h>
1220 int main(int argc, char **argv)
1221 {
1222   struct bitmask *mask = numa_parse_nodestring(NULL);
1223   return mask->size == 0;
1224 }
1225 EOF
1226 if compile_prog "" "" "libnuma api"; then
1227   libnuma_v2="yes"
1228 fi
1229 print_config "libnuma v2" "$libnuma_v2"
1230 fi
1231
1232 ##########################################
1233 # strsep() probe
1234 if test "$strsep" != "yes" ; then
1235   strsep="no"
1236 fi
1237 cat > $TMPC << EOF
1238 #include <string.h>
1239 int main(int argc, char **argv)
1240 {
1241   static char *string = "This is a string";
1242   strsep(&string, "needle");
1243   return 0;
1244 }
1245 EOF
1246 if compile_prog "" "" "strsep"; then
1247   strsep="yes"
1248 fi
1249 print_config "strsep" "$strsep"
1250
1251 ##########################################
1252 # strcasestr() probe
1253 if test "$strcasestr" != "yes" ; then
1254   strcasestr="no"
1255 fi
1256 cat > $TMPC << EOF
1257 #include <string.h>
1258 int main(int argc, char **argv)
1259 {
1260   return strcasestr(argv[0], argv[1]) != NULL;
1261 }
1262 EOF
1263 if compile_prog "" "" "strcasestr"; then
1264   strcasestr="yes"
1265 fi
1266 print_config "strcasestr" "$strcasestr"
1267
1268 ##########################################
1269 # strlcat() probe
1270 if test "$strlcat" != "yes" ; then
1271   strlcat="no"
1272 fi
1273 cat > $TMPC << EOF
1274 #include <string.h>
1275 int main(int argc, char **argv)
1276 {
1277   static char dst[64];
1278   static char *string = "This is a string";
1279   memset(dst, 0, sizeof(dst));
1280   strlcat(dst, string, sizeof(dst));
1281   return 0;
1282 }
1283 EOF
1284 if compile_prog "" "" "strlcat"; then
1285   strlcat="yes"
1286 fi
1287 print_config "strlcat" "$strlcat"
1288
1289 ##########################################
1290 # getopt_long_only() probe
1291 if test "$getopt_long_only" != "yes" ; then
1292   getopt_long_only="no"
1293 fi
1294 cat > $TMPC << EOF
1295 #include <unistd.h>
1296 #include <stdio.h>
1297 #include <getopt.h>
1298 int main(int argc, char **argv)
1299 {
1300   int c = getopt_long_only(argc, argv, NULL, NULL, NULL);
1301   return c;
1302 }
1303 EOF
1304 if compile_prog "" "" "getopt_long_only"; then
1305   getopt_long_only="yes"
1306 fi
1307 print_config "getopt_long_only()" "$getopt_long_only"
1308
1309 ##########################################
1310 # inet_aton() probe
1311 if test "$inet_aton" != "yes" ; then
1312   inet_aton="no"
1313 fi
1314 cat > $TMPC << EOF
1315 #include <sys/socket.h>
1316 #include <arpa/inet.h>
1317 #include <stdio.h>
1318 int main(int argc, char **argv)
1319 {
1320   struct in_addr in;
1321   return inet_aton(NULL, &in);
1322 }
1323 EOF
1324 if compile_prog "" "" "inet_aton"; then
1325   inet_aton="yes"
1326 fi
1327 print_config "inet_aton" "$inet_aton"
1328
1329 ##########################################
1330 # socklen_t probe
1331 if test "$socklen_t" != "yes" ; then
1332   socklen_t="no"
1333 fi
1334 cat > $TMPC << EOF
1335 #include <sys/socket.h>
1336 int main(int argc, char **argv)
1337 {
1338   socklen_t len = 0;
1339   return len;
1340 }
1341 EOF
1342 if compile_prog "" "" "socklen_t"; then
1343   socklen_t="yes"
1344 fi
1345 print_config "socklen_t" "$socklen_t"
1346
1347 ##########################################
1348 # Whether or not __thread is supported for TLS
1349 if test "$tls_thread" != "yes" ; then
1350   tls_thread="no"
1351 fi
1352 cat > $TMPC << EOF
1353 #include <stdio.h>
1354 static __thread int ret;
1355 int main(int argc, char **argv)
1356 {
1357   return ret;
1358 }
1359 EOF
1360 if compile_prog "" "" "__thread"; then
1361   tls_thread="yes"
1362 fi
1363 print_config "__thread" "$tls_thread"
1364
1365 ##########################################
1366 # Check if we have required gtk/glib support for gfio
1367 if test "$gfio" != "yes" ; then
1368   gfio="no"
1369 fi
1370 if test "$gfio_check" = "yes" ; then
1371   cat > $TMPC << EOF
1372 #include <glib.h>
1373 #include <cairo.h>
1374 #include <gtk/gtk.h>
1375 int main(void)
1376 {
1377   gdk_threads_enter();
1378   gdk_threads_leave();
1379
1380   return GTK_CHECK_VERSION(2, 18, 0) ? 0 : 1; /* 0 on success */
1381 }
1382 EOF
1383 GTK_CFLAGS=$(${cross_prefix}pkg-config --cflags gtk+-2.0 gthread-2.0)
1384 ORG_LDFLAGS=$LDFLAGS
1385 LDFLAGS=$(echo $LDFLAGS | sed s/"-static"//g)
1386 if test "$?" != "0" ; then
1387   echo "configure: gtk and gthread not found"
1388   exit 1
1389 fi
1390 GTK_LIBS=$(${cross_prefix}pkg-config --libs gtk+-2.0 gthread-2.0)
1391 if test "$?" != "0" ; then
1392   echo "configure: gtk and gthread not found"
1393   exit 1
1394 fi
1395 if ! ${cross_prefix}pkg-config --atleast-version 2.18.0 gtk+-2.0; then
1396   echo "GTK found, but need version 2.18 or higher"
1397   gfio="no"
1398 else
1399   if compile_prog "$GTK_CFLAGS" "$GTK_LIBS" "gfio" ; then
1400     gfio="yes"
1401     GFIO_LIBS="$LIBS $GTK_LIBS"
1402     CFLAGS="$CFLAGS $GTK_CFLAGS"
1403   else
1404     echo "Please install gtk and gdk libraries"
1405     gfio="no"
1406   fi
1407 fi
1408 LDFLAGS=$ORG_LDFLAGS
1409 fi
1410
1411 if test "$gfio_check" = "yes" ; then
1412   print_config "gtk 2.18 or higher" "$gfio"
1413 fi
1414
1415 ##########################################
1416 # Check whether we have getrusage(RUSAGE_THREAD)
1417 if test "$rusage_thread" != "yes" ; then
1418   rusage_thread="no"
1419 fi
1420 cat > $TMPC << EOF
1421 #include <sys/time.h>
1422 #include <sys/resource.h>
1423 int main(int argc, char **argv)
1424 {
1425   struct rusage ru;
1426   getrusage(RUSAGE_THREAD, &ru);
1427   return 0;
1428 }
1429 EOF
1430 if compile_prog "" "" "RUSAGE_THREAD"; then
1431   rusage_thread="yes"
1432 fi
1433 print_config "RUSAGE_THREAD" "$rusage_thread"
1434
1435 ##########################################
1436 # Check whether we have SCHED_IDLE
1437 if test "$sched_idle" != "yes" ; then
1438   sched_idle="no"
1439 fi
1440 cat > $TMPC << EOF
1441 #include <sched.h>
1442 int main(int argc, char **argv)
1443 {
1444   struct sched_param p;
1445   return sched_setscheduler(0, SCHED_IDLE, &p);
1446 }
1447 EOF
1448 if compile_prog "" "" "SCHED_IDLE"; then
1449   sched_idle="yes"
1450 fi
1451 print_config "SCHED_IDLE" "$sched_idle"
1452
1453 ##########################################
1454 # Check whether we have TCP_NODELAY
1455 if test "$tcp_nodelay" != "yes" ; then
1456   tcp_nodelay="no"
1457 fi
1458 cat > $TMPC << EOF
1459 #include <stdio.h>
1460 #include <sys/types.h>
1461 #include <sys/socket.h>
1462 #include <netinet/tcp.h>
1463 int main(int argc, char **argv)
1464 {
1465   return getsockopt(0, 0, TCP_NODELAY, NULL, NULL);
1466 }
1467 EOF
1468 if compile_prog "" "" "TCP_NODELAY"; then
1469   tcp_nodelay="yes"
1470 fi
1471 print_config "TCP_NODELAY" "$tcp_nodelay"
1472
1473 ##########################################
1474 # Check whether we have SO_SNDBUF
1475 if test "$window_size" != "yes" ; then
1476   window_size="no"
1477 fi
1478 cat > $TMPC << EOF
1479 #include <stdio.h>
1480 #include <sys/types.h>
1481 #include <sys/socket.h>
1482 #include <netinet/tcp.h>
1483 int main(int argc, char **argv)
1484 {
1485   setsockopt(0, SOL_SOCKET, SO_SNDBUF, NULL, 0);
1486   setsockopt(0, SOL_SOCKET, SO_RCVBUF, NULL, 0);
1487 }
1488 EOF
1489 if compile_prog "" "" "SO_SNDBUF"; then
1490   window_size="yes"
1491 fi
1492 print_config "Net engine window_size" "$window_size"
1493
1494 ##########################################
1495 # Check whether we have TCP_MAXSEG
1496 if test "$mss" != "yes" ; then
1497   mss="no"
1498 fi
1499 cat > $TMPC << EOF
1500 #include <stdio.h>
1501 #include <sys/types.h>
1502 #include <sys/socket.h>
1503 #include <netinet/tcp.h>
1504 #include <arpa/inet.h>
1505 #include <netinet/in.h>
1506 int main(int argc, char **argv)
1507 {
1508   return setsockopt(0, IPPROTO_TCP, TCP_MAXSEG, NULL, 0);
1509 }
1510 EOF
1511 if compile_prog "" "" "TCP_MAXSEG"; then
1512   mss="yes"
1513 fi
1514 print_config "TCP_MAXSEG" "$mss"
1515
1516 ##########################################
1517 # Check whether we have RLIMIT_MEMLOCK
1518 if test "$rlimit_memlock" != "yes" ; then
1519   rlimit_memlock="no"
1520 fi
1521 cat > $TMPC << EOF
1522 #include <sys/time.h>
1523 #include <sys/resource.h>
1524 int main(int argc, char **argv)
1525 {
1526   struct rlimit rl;
1527   return getrlimit(RLIMIT_MEMLOCK, &rl);
1528 }
1529 EOF
1530 if compile_prog "" "" "RLIMIT_MEMLOCK"; then
1531   rlimit_memlock="yes"
1532 fi
1533 print_config "RLIMIT_MEMLOCK" "$rlimit_memlock"
1534
1535 ##########################################
1536 # Check whether we have pwritev/preadv
1537 if test "$pwritev" != "yes" ; then
1538   pwritev="no"
1539 fi
1540 cat > $TMPC << EOF
1541 #include <stdio.h>
1542 #include <sys/uio.h>
1543 int main(int argc, char **argv)
1544 {
1545   return pwritev(0, NULL, 1, 0) + preadv(0, NULL, 1, 0);
1546 }
1547 EOF
1548 if compile_prog "" "" "pwritev"; then
1549   pwritev="yes"
1550 fi
1551 print_config "pwritev/preadv" "$pwritev"
1552
1553 ##########################################
1554 # Check whether we have pwritev2/preadv2
1555 if test "$pwritev2" != "yes" ; then
1556   pwritev2="no"
1557 fi
1558 cat > $TMPC << EOF
1559 #include <stdio.h>
1560 #include <sys/uio.h>
1561 int main(int argc, char **argv)
1562 {
1563   return pwritev2(0, NULL, 1, 0, 0) + preadv2(0, NULL, 1, 0, 0);
1564 }
1565 EOF
1566 if compile_prog "" "" "pwritev2"; then
1567   pwritev2="yes"
1568 fi
1569 print_config "pwritev2/preadv2" "$pwritev2"
1570
1571 ##########################################
1572 # Check whether we have the required functions for ipv6
1573 if test "$ipv6" != "yes" ; then
1574   ipv6="no"
1575 fi
1576 cat > $TMPC << EOF
1577 #include <sys/types.h>
1578 #include <sys/socket.h>
1579 #include <netinet/in.h>
1580 #include <netdb.h>
1581 #include <stdio.h>
1582 int main(int argc, char **argv)
1583 {
1584   struct addrinfo hints;
1585   struct in6_addr addr;
1586   int ret;
1587
1588   ret = getaddrinfo(NULL, NULL, &hints, NULL);
1589   freeaddrinfo(NULL);
1590   printf("%s\n", gai_strerror(ret));
1591   addr = in6addr_any;
1592   return 0;
1593 }
1594 EOF
1595 if compile_prog "" "" "ipv6"; then
1596   ipv6="yes"
1597 fi
1598 print_config "IPv6 helpers" "$ipv6"
1599
1600 ##########################################
1601 # check for http
1602 if test "$http" != "yes" ; then
1603   http="no"
1604 fi
1605 # check for openssl >= 1.1.0, which uses an opaque HMAC_CTX pointer
1606 cat > $TMPC << EOF
1607 #include <curl/curl.h>
1608 #include <openssl/hmac.h>
1609
1610 int main(int argc, char **argv)
1611 {
1612   CURL *curl;
1613   HMAC_CTX *ctx;
1614
1615   curl = curl_easy_init();
1616   curl_easy_cleanup(curl);
1617
1618   ctx = HMAC_CTX_new();
1619   HMAC_CTX_reset(ctx);
1620   HMAC_CTX_free(ctx);
1621   return 0;
1622 }
1623 EOF
1624 # openssl < 1.1.0 uses the HMAC_CTX type directly
1625 cat > $TMPC2 << EOF
1626 #include <curl/curl.h>
1627 #include <openssl/hmac.h>
1628
1629 int main(int argc, char **argv)
1630 {
1631   CURL *curl;
1632   HMAC_CTX ctx;
1633
1634   curl = curl_easy_init();
1635   curl_easy_cleanup(curl);
1636
1637   HMAC_CTX_init(&ctx);
1638   HMAC_CTX_cleanup(&ctx);
1639   return 0;
1640 }
1641 EOF
1642 if test "$disable_http" != "yes"; then
1643   HTTP_LIBS="-lcurl -lssl -lcrypto"
1644   if compile_prog "" "$HTTP_LIBS" "curl-new-ssl"; then
1645     output_sym "CONFIG_HAVE_OPAQUE_HMAC_CTX"
1646     http="yes"
1647     LIBS="$HTTP_LIBS $LIBS"
1648   elif mv $TMPC2 $TMPC && compile_prog "" "$HTTP_LIBS" "curl-old-ssl"; then
1649     http="yes"
1650     LIBS="$HTTP_LIBS $LIBS"
1651   fi
1652 fi
1653 print_config "http engine" "$http"
1654
1655 ##########################################
1656 # check for rados
1657 if test "$rados" != "yes" ; then
1658   rados="no"
1659 fi
1660 cat > $TMPC << EOF
1661 #include <rados/librados.h>
1662
1663 int main(int argc, char **argv)
1664 {
1665   rados_t cluster;
1666   rados_ioctx_t io_ctx;
1667   const char cluster_name[] = "ceph";
1668   const char user_name[] = "client.admin";
1669   const char pool[] = "rados";
1670
1671   /* The rados_create2 signature required was only introduced in ceph 0.65 */
1672   rados_create2(&cluster, cluster_name, user_name, 0);
1673   rados_ioctx_create(cluster, pool, &io_ctx);
1674
1675   return 0;
1676 }
1677 EOF
1678 if test "$disable_rados" != "yes"  && compile_prog "" "-lrados" "rados"; then
1679   LIBS="-lrados $LIBS"
1680   rados="yes"
1681 fi
1682 print_config "Rados engine" "$rados"
1683
1684 ##########################################
1685 # check for rbd
1686 if test "$rbd" != "yes" ; then
1687   rbd="no"
1688 fi
1689 cat > $TMPC << EOF
1690 #include <rbd/librbd.h>
1691
1692 int main(int argc, char **argv)
1693 {
1694   rados_t cluster;
1695   rados_ioctx_t io_ctx;
1696   const char cluster_name[] = "ceph";
1697   const char user_name[] = "client.admin";
1698   const char pool[] = "rbd";
1699   int major, minor, extra;
1700
1701   rbd_version(&major, &minor, &extra);
1702   /* The rados_create2 signature required was only introduced in ceph 0.65 */
1703   rados_create2(&cluster, cluster_name, user_name, 0);
1704   rados_ioctx_create(cluster, pool, &io_ctx);
1705
1706   return 0;
1707 }
1708 EOF
1709 if test "$disable_rbd" != "yes"  && compile_prog "" "-lrbd -lrados" "rbd"; then
1710   LIBS="-lrbd -lrados $LIBS"
1711   rbd="yes"
1712 fi
1713 print_config "Rados Block Device engine" "$rbd"
1714
1715 ##########################################
1716 # check for rbd_poll
1717 if test "$rbd_poll" != "yes" ; then
1718   rbd_poll="no"
1719 fi
1720 if test "$rbd" = "yes"; then
1721 cat > $TMPC << EOF
1722 #include <rbd/librbd.h>
1723 #include <sys/eventfd.h>
1724
1725 int main(int argc, char **argv)
1726 {
1727   rbd_image_t image;
1728   rbd_completion_t comp;
1729
1730   int fd = eventfd(0, EFD_NONBLOCK);
1731   rbd_set_image_notification(image, fd, EVENT_TYPE_EVENTFD);
1732   rbd_poll_io_events(image, comp, 1);
1733
1734   return 0;
1735 }
1736 EOF
1737 if compile_prog "" "-lrbd -lrados" "rbd"; then
1738   rbd_poll="yes"
1739 fi
1740 print_config "rbd_poll" "$rbd_poll"
1741 fi
1742
1743 ##########################################
1744 # check for rbd_invalidate_cache()
1745 if test "$rbd_inval" != "yes" ; then
1746   rbd_inval="no"
1747 fi
1748 if test "$rbd" = "yes"; then
1749 cat > $TMPC << EOF
1750 #include <rbd/librbd.h>
1751
1752 int main(int argc, char **argv)
1753 {
1754   rbd_image_t image;
1755
1756   return rbd_invalidate_cache(image);
1757 }
1758 EOF
1759 if compile_prog "" "-lrbd -lrados" "rbd"; then
1760   rbd_inval="yes"
1761 fi
1762 print_config "rbd_invalidate_cache" "$rbd_inval"
1763 fi
1764
1765 ##########################################
1766 # Check whether we have setvbuf
1767 if test "$setvbuf" != "yes" ; then
1768   setvbuf="no"
1769 fi
1770 cat > $TMPC << EOF
1771 #include <stdio.h>
1772 int main(int argc, char **argv)
1773 {
1774   FILE *f = NULL;
1775   char buf[80];
1776   setvbuf(f, buf, _IOFBF, sizeof(buf));
1777   return 0;
1778 }
1779 EOF
1780 if compile_prog "" "" "setvbuf"; then
1781   setvbuf="yes"
1782 fi
1783 print_config "setvbuf" "$setvbuf"
1784
1785 ##########################################
1786 # check for gfapi
1787 if test "$gfapi" != "yes" ; then
1788   gfapi="no"
1789 fi
1790 cat > $TMPC << EOF
1791 #include <glusterfs/api/glfs.h>
1792
1793 int main(int argc, char **argv)
1794 {
1795   glfs_t *g = glfs_new("foo");
1796
1797   return 0;
1798 }
1799 EOF
1800 if test "$disable_gfapi" != "yes"  && compile_prog "" "-lgfapi -lglusterfs" "gfapi"; then
1801   LIBS="-lgfapi -lglusterfs $LIBS"
1802   gfapi="yes"
1803 fi
1804 print_config "Gluster API engine" "$gfapi"
1805
1806 ##########################################
1807 # check for gfapi fadvise support, initialize with "no" only if $gfapi is set to "yes"
1808 if test "$gfapi" = "yes" ; then
1809 gf_fadvise="no"
1810 cat > $TMPC << EOF
1811 #include <glusterfs/api/glfs.h>
1812
1813 int main(int argc, char **argv)
1814 {
1815   struct glfs_fd *fd;
1816   int ret = glfs_fadvise(fd, 0, 0, 1);
1817
1818   return 0;
1819 }
1820 EOF
1821 if compile_prog "" "-lgfapi -lglusterfs" "gfapi"; then
1822   gf_fadvise="yes"
1823 fi
1824 print_config "Gluster API use fadvise" "$gf_fadvise"
1825 fi
1826
1827 ##########################################
1828 # check for newer gfapi
1829 if test "$gfapi" = "yes" ; then
1830 gf_new="no"
1831 cat > $TMPC << EOF
1832 #include <glusterfs/api/glfs.h>
1833
1834 int main(int argc, char **argv)
1835 {
1836   return glfs_fsync(NULL, NULL, NULL) && glfs_ftruncate(NULL, 0, NULL, NULL);
1837 }
1838 EOF
1839 if compile_prog "" "-lgfapi -lglusterfs" "gf new api"; then
1840   gf_new="yes"
1841 fi
1842 print_config "Gluster new API" "$gf_new"
1843 fi
1844
1845 ##########################################
1846 # check for gfapi trim support
1847 if test "$gf_trim" != "yes" ; then
1848   gf_trim="no"
1849 fi
1850 if test "$gfapi" = "yes" ; then
1851 cat > $TMPC << EOF
1852 #include <glusterfs/api/glfs.h>
1853
1854 int main(int argc, char **argv)
1855 {
1856   return glfs_discard_async(NULL, 0, 0);
1857 }
1858 EOF
1859 if compile_prog "" "-lgfapi -lglusterfs" "gf trim"; then
1860   gf_trim="yes"
1861 fi
1862 print_config "Gluster API trim support" "$gf_trim"
1863 fi
1864
1865 ##########################################
1866 # Check if we support stckf on s390
1867 if test "$s390_z196_facilities" != "yes" ; then
1868   s390_z196_facilities="no"
1869 fi
1870 cat > $TMPC << EOF
1871 #define STFLE_BITS_Z196 45 /* various z196 facilities ... */
1872 int main(int argc, char **argv)
1873 {
1874     /* We want just 1 double word to be returned.  */
1875     register unsigned long reg0 asm("0") = 0;
1876     unsigned long stfle_bits;
1877     asm volatile(".machine push"        "\n\t"
1878                  ".machine \"z9-109\""  "\n\t"
1879                  "stfle %0"             "\n\t"
1880                  ".machine pop"         "\n"
1881                  : "=QS" (stfle_bits), "+d" (reg0)
1882                  : : "cc");
1883
1884     if ((stfle_bits & (1UL << (63 - STFLE_BITS_Z196))) != 0)
1885       return 0;
1886     else
1887       return -1;
1888 }
1889 EOF
1890 if compile_prog "" "" "s390_z196_facilities"; then
1891   $TMPE
1892   if [ $? -eq 0 ]; then
1893         s390_z196_facilities="yes"
1894   fi
1895 fi
1896 print_config "s390_z196_facilities" "$s390_z196_facilities"
1897
1898 ##########################################
1899 # Check if we have required environment variables configured for libhdfs
1900 if test "$libhdfs" = "yes" ; then
1901   hdfs_conf_error=0
1902   if test "$JAVA_HOME" = "" ; then
1903     echo "configure: JAVA_HOME should be defined to jdk/jvm path"
1904     hdfs_conf_error=1
1905   fi
1906   if test "$FIO_LIBHDFS_INCLUDE" = "" ; then
1907     echo "configure: FIO_LIBHDFS_INCLUDE should be defined to libhdfs inlude path"
1908     hdfs_conf_error=1
1909   fi
1910   if test "$FIO_LIBHDFS_LIB" = "" ; then
1911     echo "configure: FIO_LIBHDFS_LIB should be defined to libhdfs library path"
1912     hdfs_conf_error=1
1913   fi
1914   if test "$hdfs_conf_error" = "1" ; then
1915     exit 1
1916   fi
1917   FIO_HDFS_CPU=$cpu
1918   if test "$FIO_HDFS_CPU" = "x86_64" ; then
1919     FIO_HDFS_CPU="amd64"
1920   fi
1921 fi
1922 print_config "HDFS engine" "$libhdfs"
1923
1924 ##########################################
1925 # Check whether we have MTD
1926 if test "$mtd" != "yes" ; then
1927   mtd="no"
1928 fi
1929 cat > $TMPC << EOF
1930 #include <string.h>
1931 #include <mtd/mtd-user.h>
1932 #include <sys/ioctl.h>
1933 int main(int argc, char **argv)
1934 {
1935   struct mtd_write_req ops;
1936   struct mtd_info_user info;
1937   memset(&ops, 0, sizeof(ops));
1938   info.type = MTD_MLCNANDFLASH;
1939   return ioctl(0, MEMGETINFO, &info);
1940 }
1941 EOF
1942 if compile_prog "" "" "mtd"; then
1943   mtd="yes"
1944 fi
1945 print_config "MTD" "$mtd"
1946
1947 ##########################################
1948 # Check whether we have libpmem
1949 if test "$libpmem" != "yes" ; then
1950   libpmem="no"
1951 fi
1952 cat > $TMPC << EOF
1953 #include <libpmem.h>
1954 int main(int argc, char **argv)
1955 {
1956   int rc;
1957   rc = pmem_is_pmem(0, 0);
1958   return 0;
1959 }
1960 EOF
1961 if compile_prog "" "-lpmem" "libpmem"; then
1962   libpmem="yes"
1963   LIBS="-lpmem $LIBS"
1964 fi
1965 print_config "libpmem" "$libpmem"
1966
1967 ##########################################
1968 # Check whether we have libpmemblk
1969 # libpmem is a prerequisite
1970 if test "$libpmemblk" != "yes" ; then
1971   libpmemblk="no"
1972 fi
1973 if test "$libpmem" = "yes"; then
1974   cat > $TMPC << EOF
1975 #include <libpmemblk.h>
1976 int main(int argc, char **argv)
1977 {
1978   PMEMblkpool *pbp;
1979   pbp = pmemblk_open("", 0);
1980   return 0;
1981 }
1982 EOF
1983   if compile_prog "" "-lpmemblk" "libpmemblk"; then
1984     libpmemblk="yes"
1985     LIBS="-lpmemblk $LIBS"
1986   fi
1987 fi
1988 print_config "libpmemblk" "$libpmemblk"
1989
1990 # Choose the ioengines
1991 if test "$libpmem" = "yes" && test "$disable_pmem" = "no"; then
1992   pmem="yes"
1993   devdax="yes"
1994   if test "$libpmemblk" = "yes"; then
1995     pmemblk="yes"
1996   fi
1997 fi
1998
1999 ##########################################
2000 # Report whether pmemblk engine is enabled
2001 print_config "PMDK pmemblk engine" "$pmemblk"
2002
2003 ##########################################
2004 # Report whether dev-dax engine is enabled
2005 print_config "PMDK dev-dax engine" "$devdax"
2006
2007 ##########################################
2008 # Report whether libpmem engine is enabled
2009 print_config "PMDK libpmem engine" "$pmem"
2010
2011 ##########################################
2012 # Check whether we support DDN's IME
2013 if test "$libime" != "yes" ; then
2014   libime="no"
2015 fi
2016 cat > $TMPC << EOF
2017 #include <ime_native.h>
2018 int main(int argc, char **argv)
2019 {
2020   int rc;
2021   ime_native_init();
2022   rc = ime_native_finalize();
2023   return 0;
2024 }
2025 EOF
2026 if compile_prog "-I${ime_path}/include" "-L${ime_path}/lib -lim_client" "libime"; then
2027   libime="yes"
2028   CFLAGS="-I${ime_path}/include $CFLAGS"
2029   LDFLAGS="-Wl,-rpath ${ime_path}/lib -L${ime_path}/lib $LDFLAGS"
2030   LIBS="-lim_client $LIBS"
2031 fi
2032 print_config "DDN's Infinite Memory Engine" "$libime"
2033
2034 ##########################################
2035 # Check if we have required environment variables configured for libiscsi
2036 if test "$libiscsi" = "yes" ; then
2037   if $(pkg-config --atleast-version=1.9.0 libiscsi); then
2038     libiscsi="yes"
2039     libiscsi_cflags=$(pkg-config --cflags libiscsi)
2040     libiscsi_libs=$(pkg-config --libs libiscsi)
2041   else
2042     if test "$libiscsi" = "yes" ; then
2043       echo "libiscsi" "Install libiscsi >= 1.9.0"
2044     fi
2045     libiscsi="no"
2046   fi
2047 fi
2048 print_config "iscsi engine" "$libiscsi"
2049
2050 ##########################################
2051 # Check if we have libnbd (for NBD support).
2052 minimum_libnbd=0.9.8
2053 if test "$libnbd" = "yes" ; then
2054   if $(pkg-config --atleast-version=$minimum_libnbd libnbd); then
2055     libnbd="yes"
2056     libnbd_cflags=$(pkg-config --cflags libnbd)
2057     libnbd_libs=$(pkg-config --libs libnbd)
2058   else
2059     if test "$libnbd" = "yes" ; then
2060       echo "libnbd" "Install libnbd >= $minimum_libnbd"
2061     fi
2062     libnbd="no"
2063   fi
2064 fi
2065 print_config "NBD engine" "$libnbd"
2066
2067 ##########################################
2068 # Check if we have lex/yacc available
2069 yacc="no"
2070 yacc_is_bison="no"
2071 lex="no"
2072 arith="no"
2073 if test "$disable_lex" = "no" || test -z "$disable_lex" ; then
2074 if test "$targetos" != "SunOS" ; then
2075 LEX=$(which lex 2> /dev/null)
2076 if test -x "$LEX" ; then
2077   lex="yes"
2078 fi
2079 YACC=$(which bison 2> /dev/null)
2080 if test -x "$YACC" ; then
2081   yacc="yes"
2082   yacc_is_bison="yes"
2083 else
2084   YACC=$(which yacc 2> /dev/null)
2085   if test -x "$YACC" ; then
2086     yacc="yes"
2087   fi
2088 fi
2089 if test "$yacc" = "yes" && test "$lex" = "yes" ; then
2090   arith="yes"
2091 fi
2092
2093 if test "$arith" = "yes" ; then
2094 cat > $TMPC << EOF
2095 extern int yywrap(void);
2096
2097 int main(int argc, char **argv)
2098 {
2099   yywrap();
2100   return 0;
2101 }
2102 EOF
2103 if compile_prog "" "-ll" "lex"; then
2104   LIBS="-ll $LIBS"
2105 else
2106   arith="no"
2107 fi
2108 fi
2109 fi
2110 fi
2111
2112 # Check if lex fails using -o
2113 if test "$arith" = "yes" ; then
2114 if test "$force_no_lex_o" = "yes" ; then
2115   lex_use_o="no"
2116 else
2117 $LEX -o lex.yy.c exp/expression-parser.l 2> /dev/null
2118 if test "$?" = "0" ; then
2119   lex_use_o="yes"
2120 else
2121   lex_use_o="no"
2122 fi
2123 fi
2124 fi
2125
2126 print_config "lex/yacc for arithmetic" "$arith"
2127
2128 ##########################################
2129 # Check whether we have setmntent/getmntent
2130 if test "$getmntent" != "yes" ; then
2131   getmntent="no"
2132 fi
2133 cat > $TMPC << EOF
2134 #include <stdio.h>
2135 #include <mntent.h>
2136 int main(int argc, char **argv)
2137 {
2138   FILE *mtab = setmntent(NULL, "r");
2139   struct mntent *mnt = getmntent(mtab);
2140   endmntent(mtab);
2141   return 0;
2142 }
2143 EOF
2144 if compile_prog "" "" "getmntent"; then
2145   getmntent="yes"
2146 fi
2147 print_config "getmntent" "$getmntent"
2148
2149 ##########################################
2150 # Check whether we have getmntinfo
2151 # These are originally added for BSDs, but may also work
2152 # on other operating systems with getmntinfo(3).
2153
2154 # getmntinfo(3) for FreeBSD/DragonFlyBSD/OpenBSD.
2155 # Note that NetBSD needs -Werror to catch warning as error.
2156 if test "$getmntinfo" != "yes" ; then
2157   getmntinfo="no"
2158 fi
2159 cat > $TMPC << EOF
2160 #include <stdio.h>
2161 #include <sys/param.h>
2162 #include <sys/mount.h>
2163 int main(int argc, char **argv)
2164 {
2165   struct statfs *st;
2166   return getmntinfo(&st, MNT_NOWAIT);
2167 }
2168 EOF
2169 if compile_prog "-Werror" "" "getmntinfo"; then
2170   getmntinfo="yes"
2171 fi
2172 print_config "getmntinfo" "$getmntinfo"
2173
2174 # getmntinfo(3) for NetBSD.
2175 if test "$getmntinfo_statvfs" != "yes" ; then
2176   getmntinfo_statvfs="no"
2177 fi
2178 cat > $TMPC << EOF
2179 #include <stdio.h>
2180 #include <sys/statvfs.h>
2181 int main(int argc, char **argv)
2182 {
2183   struct statvfs *st;
2184   return getmntinfo(&st, MNT_NOWAIT);
2185 }
2186 EOF
2187 # Skip the test if the one with statfs arg is detected.
2188 if test "$getmntinfo" != "yes" && compile_prog "-Werror" "" "getmntinfo_statvfs"; then
2189   getmntinfo_statvfs="yes"
2190   print_config "getmntinfo_statvfs" "$getmntinfo_statvfs"
2191 fi
2192
2193 ##########################################
2194 # Check whether we have _Static_assert
2195 if test "$static_assert" != "yes" ; then
2196   static_assert="no"
2197 fi
2198 cat > $TMPC << EOF
2199 #include <assert.h>
2200 #include <stdlib.h>
2201 #include <stddef.h>
2202
2203 struct foo {
2204   int a, b;
2205 };
2206
2207 int main(int argc, char **argv)
2208 {
2209   _Static_assert(offsetof(struct foo, a) == 0 , "Check");
2210   return 0 ;
2211 }
2212 EOF
2213 if compile_prog "" "" "static_assert"; then
2214     static_assert="yes"
2215 fi
2216 print_config "Static Assert" "$static_assert"
2217
2218 ##########################################
2219 # Check whether we have bool / stdbool.h
2220 if test "$have_bool" != "yes" ; then
2221   have_bool="no"
2222 fi
2223 cat > $TMPC << EOF
2224 #include <stdbool.h>
2225 int main(int argc, char **argv)
2226 {
2227   bool var = true;
2228   return var != false;
2229 }
2230 EOF
2231 if compile_prog "" "" "bool"; then
2232   have_bool="yes"
2233 fi
2234 print_config "bool" "$have_bool"
2235
2236 ##########################################
2237 # Check whether we have strndup()
2238 strndup="no"
2239 cat > $TMPC << EOF
2240 #include <string.h>
2241 #include <stdlib.h>
2242 int main(int argc, char **argv)
2243 {
2244   char *res = strndup("test string", 8);
2245
2246   free(res);
2247   return 0;
2248 }
2249 EOF
2250 if compile_prog "" "" "strndup"; then
2251   strndup="yes"
2252 fi
2253 print_config "strndup" "$strndup"
2254
2255 ##########################################
2256 # <valgrind/drd.h> probe
2257 # Note: presence of <valgrind/drd.h> implies that <valgrind/valgrind.h> is
2258 # also available but not the other way around.
2259 if test "$valgrind_dev" != "yes" ; then
2260   valgrind_dev="no"
2261 fi
2262 cat > $TMPC << EOF
2263 #include <valgrind/drd.h>
2264 int main(int argc, char **argv)
2265 {
2266   return 0;
2267 }
2268 EOF
2269 if compile_prog "" "" "valgrind_dev"; then
2270   valgrind_dev="yes"
2271 fi
2272 print_config "Valgrind headers" "$valgrind_dev"
2273
2274 ##########################################
2275 # <linux/blkzoned.h> probe
2276 if test "$linux_blkzoned" != "yes" ; then
2277   linux_blkzoned="no"
2278 fi
2279 cat > $TMPC << EOF
2280 #include <linux/blkzoned.h>
2281 int main(int argc, char **argv)
2282 {
2283   return 0;
2284 }
2285 EOF
2286 if compile_prog "" "" "linux_blkzoned"; then
2287   linux_blkzoned="yes"
2288 fi
2289 print_config "Zoned block device support" "$linux_blkzoned"
2290
2291 ##########################################
2292 # check march=armv8-a+crc+crypto
2293 if test "$march_armv8_a_crc_crypto" != "yes" ; then
2294   march_armv8_a_crc_crypto="no"
2295 fi
2296 if test "$cpu" = "arm64" ; then
2297   cat > $TMPC <<EOF
2298 #include <arm_acle.h>
2299 #include <arm_neon.h>
2300 #include <sys/auxv.h>
2301
2302 int main(void)
2303 {
2304   /* Can we also do a runtime probe? */
2305 #if __linux__
2306   return getauxval(AT_HWCAP);
2307 #else
2308 # error "Don't know how to do runtime probe for ARM CRC32c"
2309 #endif
2310 }
2311 EOF
2312   if compile_prog "-march=armv8-a+crc+crypto" "" "ARM CRC32c"; then
2313     march_armv8_a_crc_crypto="yes"
2314     CFLAGS="$CFLAGS -march=armv8-a+crc+crypto"
2315     march_set="yes"
2316   fi
2317 fi
2318 print_config "march_armv8_a_crc_crypto" "$march_armv8_a_crc_crypto"
2319
2320 ##########################################
2321 # cuda probe
2322 if test "$cuda" != "yes" ; then
2323   cuda="no"
2324 fi
2325 cat > $TMPC << EOF
2326 #include <cuda.h>
2327 int main(int argc, char **argv)
2328 {
2329   return cuInit(0);
2330 }
2331 EOF
2332 if test "$enable_cuda" = "yes" && compile_prog "" "-lcuda" "cuda"; then
2333   cuda="yes"
2334   LIBS="-lcuda $LIBS"
2335 fi
2336 print_config "cuda" "$cuda"
2337
2338 ##########################################
2339 # check for cc -march=native
2340 build_native="no"
2341 cat > $TMPC << EOF
2342 int main(int argc, char **argv)
2343 {
2344   return 0;
2345 }
2346 EOF
2347 if test "$disable_native" = "no" && test "$disable_opt" != "yes" && \
2348    compile_prog "-march=native" "" "march=native"; then
2349   build_native="yes"
2350 fi
2351 print_config "Build march=native" "$build_native"
2352
2353 ##########################################
2354 # check for -lcunit
2355 if test "$cunit" != "yes" ; then
2356   cunit="no"
2357 fi
2358 cat > $TMPC << EOF
2359 #include <CUnit/CUnit.h>
2360 #include <CUnit/Basic.h>
2361 int main(void)
2362 {
2363   if (CU_initialize_registry() != CUE_SUCCESS)
2364     return CU_get_error();
2365   CU_basic_set_mode(CU_BRM_VERBOSE);
2366   CU_basic_run_tests();
2367   CU_cleanup_registry();
2368   return CU_get_error();
2369 }
2370 EOF
2371 if compile_prog "" "-lcunit" "CUnit"; then
2372   cunit="yes"
2373 fi
2374 print_config "CUnit" "$cunit"
2375
2376 ##########################################
2377 # check for __kernel_rwf_t
2378 __kernel_rwf_t="no"
2379 cat > $TMPC << EOF
2380 #include <linux/fs.h>
2381 int main(int argc, char **argv)
2382 {
2383   __kernel_rwf_t x;
2384   x = 0;
2385   return x;
2386 }
2387 EOF
2388 if compile_prog "" "" "__kernel_rwf_t"; then
2389   __kernel_rwf_t="yes"
2390 fi
2391 print_config "__kernel_rwf_t" "$__kernel_rwf_t"
2392
2393 ##########################################
2394 # check if gcc has -Wimplicit-fallthrough
2395 fallthrough="no"
2396 cat > $TMPC << EOF
2397 int main(int argc, char **argv)
2398 {
2399   return 0;
2400 }
2401 EOF
2402 if compile_prog "-Wimplicit-fallthrough" "" "-Wimplicit-fallthrough"; then
2403   fallthrough="yes"
2404 fi
2405 print_config "-Wimplicit-fallthrough" "$fallthrough"
2406
2407 ##########################################
2408 # check for MADV_HUGEPAGE support
2409 if test "$thp" != "yes" ; then
2410   thp="no"
2411 fi
2412 if test "$esx" != "yes" ; then
2413   cat > $TMPC <<EOF
2414 #include <sys/mman.h>
2415 int main(void)
2416 {
2417   return madvise(0, 0x1000, MADV_HUGEPAGE);
2418 }
2419 EOF
2420   if compile_prog "" "" "thp" ; then
2421     thp=yes
2422   else
2423     if test "$thp" = "yes" ; then
2424       feature_not_found "Transparent Huge Page" ""
2425     fi
2426     thp=no
2427   fi
2428 fi
2429 print_config "MADV_HUGEPAGE" "$thp"
2430
2431 ##########################################
2432 # check for gettid()
2433 gettid="no"
2434 cat > $TMPC << EOF
2435 #include <unistd.h>
2436 int main(int argc, char **argv)
2437 {
2438   return gettid();
2439 }
2440 EOF
2441 if compile_prog "" "" "gettid"; then
2442   gettid="yes"
2443 fi
2444 print_config "gettid" "$gettid"
2445
2446 #############################################################################
2447
2448 if test "$wordsize" = "64" ; then
2449   output_sym "CONFIG_64BIT"
2450 elif test "$wordsize" = "32" ; then
2451   output_sym "CONFIG_32BIT"
2452 else
2453   fatal "Unknown wordsize!"
2454 fi
2455 if test "$bigendian" = "yes" ; then
2456   output_sym "CONFIG_BIG_ENDIAN"
2457 else
2458   output_sym "CONFIG_LITTLE_ENDIAN"
2459 fi
2460 if test "$zlib" = "yes" ; then
2461   output_sym "CONFIG_ZLIB"
2462 fi
2463 if test "$libaio" = "yes" ; then
2464   output_sym "CONFIG_LIBAIO"
2465   if test "$libaio_uring" = "yes" ; then
2466     output_sym "CONFIG_LIBAIO_URING"
2467   fi
2468 fi
2469 if test "$posix_aio" = "yes" ; then
2470   output_sym "CONFIG_POSIXAIO"
2471 fi
2472 if test "$posix_aio_fsync" = "yes" ; then
2473   output_sym "CONFIG_POSIXAIO_FSYNC"
2474 fi
2475 if test "$posix_pshared" = "yes" ; then
2476   output_sym "CONFIG_PSHARED"
2477 fi
2478 if test "$pthread_condattr_setclock" = "yes" ; then
2479   output_sym "CONFIG_PTHREAD_CONDATTR_SETCLOCK"
2480 fi
2481 if test "$have_asprintf" = "yes" ; then
2482     output_sym "CONFIG_HAVE_ASPRINTF"
2483 fi
2484 if test "$have_vasprintf" = "yes" ; then
2485     output_sym "CONFIG_HAVE_VASPRINTF"
2486 fi
2487 if test "$linux_fallocate" = "yes" ; then
2488   output_sym "CONFIG_LINUX_FALLOCATE"
2489 fi
2490 if test "$posix_fallocate" = "yes" ; then
2491   output_sym "CONFIG_POSIX_FALLOCATE"
2492 fi
2493 if test "$fdatasync" = "yes" ; then
2494   output_sym "CONFIG_FDATASYNC"
2495 fi
2496 if test "$sync_file_range" = "yes" ; then
2497   output_sym "CONFIG_SYNC_FILE_RANGE"
2498 fi
2499 if test "$sfaa" = "yes" ; then
2500   output_sym "CONFIG_SFAA"
2501 fi
2502 if test "$sync_sync" = "yes" ; then
2503   output_sym "CONFIG_SYNC_SYNC"
2504 fi
2505 if test "$cmp_swap" = "yes" ; then
2506   output_sym "CONFIG_CMP_SWAP"
2507 fi
2508 if test "$libverbs" = "yes" -a "$rdmacm" = "yes" ; then
2509   output_sym "CONFIG_RDMA"
2510 fi
2511 if test "$clock_gettime" = "yes" ; then
2512   output_sym "CONFIG_CLOCK_GETTIME"
2513 fi
2514 if test "$clock_monotonic" = "yes" ; then
2515   output_sym "CONFIG_CLOCK_MONOTONIC"
2516 fi
2517 if test "$clock_monotonic_raw" = "yes" ; then
2518   output_sym "CONFIG_CLOCK_MONOTONIC_RAW"
2519 fi
2520 if test "$clock_monotonic_precise" = "yes" ; then
2521   output_sym "CONFIG_CLOCK_MONOTONIC_PRECISE"
2522 fi
2523 if test "$clockid_t" = "yes"; then
2524   output_sym "CONFIG_CLOCKID_T"
2525 fi
2526 if test "$gettimeofday" = "yes" ; then
2527   output_sym "CONFIG_GETTIMEOFDAY"
2528 fi
2529 if test "$posix_fadvise" = "yes" ; then
2530   output_sym "CONFIG_POSIX_FADVISE"
2531 fi
2532 if test "$linux_3arg_affinity" = "yes" ; then
2533   output_sym "CONFIG_3ARG_AFFINITY"
2534 elif test "$linux_2arg_affinity" = "yes" ; then
2535   output_sym "CONFIG_2ARG_AFFINITY"
2536 fi
2537 if test "$strsep" = "yes" ; then
2538   output_sym "CONFIG_STRSEP"
2539 fi
2540 if test "$strcasestr" = "yes" ; then
2541   output_sym "CONFIG_STRCASESTR"
2542 fi
2543 if test "$strlcat" = "yes" ; then
2544   output_sym "CONFIG_STRLCAT"
2545 fi
2546 if test "$getopt_long_only" = "yes" ; then
2547   output_sym "CONFIG_GETOPT_LONG_ONLY"
2548 fi
2549 if test "$inet_aton" = "yes" ; then
2550   output_sym "CONFIG_INET_ATON"
2551 fi
2552 if test "$socklen_t" = "yes" ; then
2553   output_sym "CONFIG_SOCKLEN_T"
2554 fi
2555 if test "$ext4_me" = "yes" ; then
2556   output_sym "CONFIG_LINUX_EXT4_MOVE_EXTENT"
2557 fi
2558 if test "$linux_splice" = "yes" ; then
2559   output_sym "CONFIG_LINUX_SPLICE"
2560 fi
2561 if test "$guasi" = "yes" ; then
2562   output_sym "CONFIG_GUASI"
2563 fi
2564 if test "$libnuma_v2" = "yes" ; then
2565   output_sym "CONFIG_LIBNUMA"
2566 fi
2567 if test "$solaris_aio" = "yes" ; then
2568   output_sym "CONFIG_SOLARISAIO"
2569 fi
2570 if test "$tls_thread" = "yes" ; then
2571   output_sym "CONFIG_TLS_THREAD"
2572 fi
2573 if test "$rusage_thread" = "yes" ; then
2574   output_sym "CONFIG_RUSAGE_THREAD"
2575 fi
2576 if test "$gfio" = "yes" ; then
2577   output_sym "CONFIG_GFIO"
2578 fi
2579 if test "$esx" = "yes" ; then
2580   output_sym "CONFIG_ESX"
2581   output_sym "CONFIG_NO_SHM"
2582 fi
2583 if test "$sched_idle" = "yes" ; then
2584   output_sym "CONFIG_SCHED_IDLE"
2585 fi
2586 if test "$tcp_nodelay" = "yes" ; then
2587   output_sym "CONFIG_TCP_NODELAY"
2588 fi
2589 if test "$window_size" = "yes" ; then
2590   output_sym "CONFIG_NET_WINDOWSIZE"
2591 fi
2592 if test "$mss" = "yes" ; then
2593   output_sym "CONFIG_NET_MSS"
2594 fi
2595 if test "$rlimit_memlock" = "yes" ; then
2596   output_sym "CONFIG_RLIMIT_MEMLOCK"
2597 fi
2598 if test "$pwritev" = "yes" ; then
2599   output_sym "CONFIG_PWRITEV"
2600 fi
2601 if test "$pwritev2" = "yes" ; then
2602   output_sym "CONFIG_PWRITEV2"
2603 fi
2604 if test "$ipv6" = "yes" ; then
2605   output_sym "CONFIG_IPV6"
2606 fi
2607 if test "$http" = "yes" ; then
2608   output_sym "CONFIG_HTTP"
2609 fi
2610 if test "$rados" = "yes" ; then
2611   output_sym "CONFIG_RADOS"
2612 fi
2613 if test "$rbd" = "yes" ; then
2614   output_sym "CONFIG_RBD"
2615 fi
2616 if test "$rbd_poll" = "yes" ; then
2617   output_sym "CONFIG_RBD_POLL"
2618 fi
2619 if test "$rbd_inval" = "yes" ; then
2620   output_sym "CONFIG_RBD_INVAL"
2621 fi
2622 if test "$setvbuf" = "yes" ; then
2623   output_sym "CONFIG_SETVBUF"
2624 fi
2625 if test "$s390_z196_facilities" = "yes" ; then
2626   output_sym "CONFIG_S390_Z196_FACILITIES"
2627   CFLAGS="$CFLAGS -march=z9-109"
2628   march_set="yes"
2629 fi
2630 if test "$gfapi" = "yes" ; then
2631   output_sym "CONFIG_GFAPI"
2632 fi
2633 if test "$gf_fadvise" = "yes" ; then
2634   output_sym "CONFIG_GF_FADVISE"
2635 fi
2636 if test "$gf_trim" = "yes" ; then
2637   output_sym "CONFIG_GF_TRIM"
2638 fi
2639 if test "$gf_new" = "yes" ; then
2640   output_sym "CONFIG_GF_NEW_API"
2641 fi
2642 if test "$libhdfs" = "yes" ; then
2643   output_sym "CONFIG_LIBHDFS"
2644   echo "FIO_HDFS_CPU=$FIO_HDFS_CPU" >> $config_host_mak
2645   echo "JAVA_HOME=$JAVA_HOME" >> $config_host_mak
2646   echo "FIO_LIBHDFS_INCLUDE=$FIO_LIBHDFS_INCLUDE" >> $config_host_mak
2647   echo "FIO_LIBHDFS_LIB=$FIO_LIBHDFS_LIB" >> $config_host_mak
2648 fi
2649 if test "$mtd" = "yes" ; then
2650   output_sym "CONFIG_MTD"
2651 fi
2652 if test "$pmemblk" = "yes" ; then
2653   output_sym "CONFIG_PMEMBLK"
2654 fi
2655 if test "$devdax" = "yes" ; then
2656   output_sym "CONFIG_LINUX_DEVDAX"
2657 fi
2658 if test "$pmem" = "yes" ; then
2659   output_sym "CONFIG_LIBPMEM"
2660 fi
2661 if test "$libime" = "yes" ; then
2662   output_sym "CONFIG_IME"
2663 fi
2664 if test "$arith" = "yes" ; then
2665   output_sym "CONFIG_ARITHMETIC"
2666   if test "$yacc_is_bison" = "yes" ; then
2667     echo "YACC=$YACC -y" >> $config_host_mak
2668   else
2669     echo "YACC=$YACC" >> $config_host_mak
2670   fi
2671   if test "$lex_use_o" = "yes" ; then
2672     echo "CONFIG_LEX_USE_O=y" >> $config_host_mak
2673   fi
2674 fi
2675 if test "$getmntent" = "yes" ; then
2676   output_sym "CONFIG_GETMNTENT"
2677 fi
2678 if test "$getmntinfo" = "yes" ; then
2679   output_sym "CONFIG_GETMNTINFO"
2680 fi
2681 if test "$getmntinfo_statvfs" = "yes" ; then
2682   output_sym "CONFIG_GETMNTINFO_STATVFS"
2683 fi
2684 if test "$static_assert" = "yes" ; then
2685   output_sym "CONFIG_STATIC_ASSERT"
2686 fi
2687 if test "$have_bool" = "yes" ; then
2688   output_sym "CONFIG_HAVE_BOOL"
2689 fi
2690 if test "$strndup" = "yes" ; then
2691   output_sym "CONFIG_HAVE_STRNDUP"
2692 fi
2693 if test "$disable_opt" = "yes" ; then
2694   output_sym "CONFIG_DISABLE_OPTIMIZATIONS"
2695 fi
2696 if test "$valgrind_dev" = "yes"; then
2697   output_sym "CONFIG_VALGRIND_DEV"
2698 fi
2699 if test "$linux_blkzoned" = "yes" ; then
2700   output_sym "CONFIG_LINUX_BLKZONED"
2701 fi
2702 if test "$zlib" = "no" ; then
2703   echo "Consider installing zlib-dev (zlib-devel, some fio features depend on it."
2704   if test "$build_static" = "yes"; then
2705     echo "Note that some distros have separate packages for static libraries."
2706   fi
2707 fi
2708 if test "$march_armv8_a_crc_crypto" = "yes" ; then
2709   output_sym "ARCH_HAVE_CRC_CRYPTO"
2710 fi
2711 if test "$cuda" = "yes" ; then
2712   output_sym "CONFIG_CUDA"
2713 fi
2714 if test "$march_set" = "no" && test "$build_native" = "yes" ; then
2715   output_sym "CONFIG_BUILD_NATIVE"
2716 fi
2717 if test "$cunit" = "yes" ; then
2718   output_sym "CONFIG_HAVE_CUNIT"
2719 fi
2720 if test "$__kernel_rwf_t" = "yes"; then
2721   output_sym "CONFIG_HAVE_KERNEL_RWF_T"
2722 fi
2723 if test "$gettid" = "yes"; then
2724   output_sym "CONFIG_HAVE_GETTID"
2725 fi
2726 if test "$fallthrough" = "yes"; then
2727   CFLAGS="$CFLAGS -Wimplicit-fallthrough"
2728 fi
2729 if test "$thp" = "yes" ; then
2730   output_sym "CONFIG_HAVE_THP"
2731 fi
2732 if test "$libiscsi" = "yes" ; then
2733   output_sym "CONFIG_LIBISCSI"
2734   echo "CONFIG_LIBISCSI=m" >> $config_host_mak
2735   echo "LIBISCSI_CFLAGS=$libiscsi_cflags" >> $config_host_mak
2736   echo "LIBISCSI_LIBS=$libiscsi_libs" >> $config_host_mak
2737 fi
2738 if test "$libnbd" = "yes" ; then
2739   output_sym "CONFIG_LIBNBD"
2740   echo "CONFIG_LIBNBD=m" >> $config_host_mak
2741   echo "LIBNBD_CFLAGS=$libnbd_cflags" >> $config_host_mak
2742   echo "LIBNBD_LIBS=$libnbd_libs" >> $config_host_mak
2743 fi
2744 cat > $TMPC << EOF
2745 int main(int argc, char **argv)
2746 {
2747   return 0;
2748 }
2749 EOF
2750 if test "$disable_tcmalloc" != "yes"  && compile_prog "" "-ltcmalloc" "tcmalloc"; then
2751   LIBS="-ltcmalloc $LIBS"
2752   tcmalloc="yes"
2753 else
2754   tcmalloc="no"
2755 fi
2756 print_config "TCMalloc support" "$tcmalloc"
2757
2758 echo "LIBS+=$LIBS" >> $config_host_mak
2759 echo "GFIO_LIBS+=$GFIO_LIBS" >> $config_host_mak
2760 echo "CFLAGS+=$CFLAGS" >> $config_host_mak
2761 echo "LDFLAGS+=$LDFLAGS" >> $config_host_mak
2762 echo "CC=$cc" >> $config_host_mak
2763 echo "BUILD_CFLAGS=$BUILD_CFLAGS $CFLAGS" >> $config_host_mak
2764 echo "INSTALL_PREFIX=$prefix" >> $config_host_mak
2765
2766 if [ `dirname $0` != "." -a ! -e Makefile ]; then
2767     cat > Makefile <<EOF
2768 SRCDIR:=`dirname $0`
2769 include \$(SRCDIR)/Makefile
2770 EOF
2771 fi