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