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