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