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