]> CyberLeo.Net >> Repos - FreeBSD/FreeBSD.git/blob - share/mk/bsd.sys.mk
zfs: merge openzfs/zfs@c3b60eded (zfs-2.1-release) into stable/13
[FreeBSD/FreeBSD.git] / share / mk / bsd.sys.mk
1 # $FreeBSD$
2 #
3 # This file contains common settings used for building FreeBSD
4 # sources.
5
6 # Enable various levels of compiler warning checks.  These may be
7 # overridden (e.g. if using a non-gcc compiler) by defining MK_WARNS=no.
8
9 # for GCC:   https://gcc.gnu.org/onlinedocs/gcc/Warning-Options.html
10 # for clang: https://clang.llvm.org/docs/DiagnosticsReference.html
11
12 .include <bsd.compiler.mk>
13
14 # the default is gnu99 for now
15 CSTD?=          gnu99
16
17 .if ${CSTD} == "c89" || ${CSTD} == "c90"
18 CFLAGS+=        -std=iso9899:1990
19 .elif ${CSTD} == "c94" || ${CSTD} == "c95"
20 CFLAGS+=        -std=iso9899:199409
21 .elif ${CSTD} == "c99"
22 CFLAGS+=        -std=iso9899:1999
23 .else # CSTD
24 CFLAGS+=        -std=${CSTD}
25 .endif # CSTD
26
27 .if !empty(CXXSTD)
28 CXXFLAGS+=      -std=${CXXSTD}
29 .endif
30
31 # This gives the Makefile we're evaluating at the top-level a chance to set
32 # WARNS.  If it doesn't do so, we may freely pull a DEFAULTWARNS if it's set
33 # and use that.  This allows us to default WARNS to 6 for src builds without
34 # needing to set the default in various Makefile.inc.
35 .if !defined(WARNS) && defined(DEFAULTWARNS)
36 WARNS=  ${DEFAULTWARNS}
37 .endif
38
39 # -pedantic is problematic because it also imposes namespace restrictions
40 #CFLAGS+=       -pedantic
41 .if defined(WARNS)
42 .if ${WARNS} >= 1
43 CWARNFLAGS+=    -Wsystem-headers
44 .if ${MK_WERROR} != "no" && ${MK_WERROR.${COMPILER_TYPE}:Uyes} != "no"
45 CWARNFLAGS+=    -Werror
46 .endif # ${MK_WERROR} != "no" && ${MK_WERROR.${COMPILER_TYPE}:Uyes} != "no"
47 .endif # WARNS >= 1
48 .if ${WARNS} >= 2
49 CWARNFLAGS+=    -Wall -Wno-format-y2k
50 .endif # WARNS >= 2
51 .if ${WARNS} >= 3
52 CWARNFLAGS+=    -W -Wno-unused-parameter -Wstrict-prototypes\
53                 -Wmissing-prototypes -Wpointer-arith
54 .endif # WARNS >= 3
55 .if ${WARNS} >= 4
56 CWARNFLAGS+=    -Wreturn-type -Wcast-qual -Wwrite-strings -Wswitch -Wshadow\
57                 -Wunused-parameter
58 .if !defined(NO_WCAST_ALIGN) && !defined(NO_WCAST_ALIGN.${COMPILER_TYPE})
59 CWARNFLAGS+=    -Wcast-align
60 .endif # !NO_WCAST_ALIGN !NO_WCAST_ALIGN.${COMPILER_TYPE}
61 .endif # WARNS >= 4
62 .if ${WARNS} >= 6
63 CWARNFLAGS+=    -Wchar-subscripts -Wnested-externs -Wredundant-decls\
64                 -Wold-style-definition
65 .if !defined(NO_WMISSING_VARIABLE_DECLARATIONS)
66 CWARNFLAGS.clang+=      -Wmissing-variable-declarations
67 .endif
68 .if !defined(NO_WTHREAD_SAFETY)
69 CWARNFLAGS.clang+=      -Wthread-safety
70 .endif
71 .endif # WARNS >= 6
72 .if ${WARNS} >= 2 && ${WARNS} <= 4
73 # XXX Delete -Wuninitialized by default for now -- the compiler doesn't
74 # XXX always get it right.
75 CWARNFLAGS+=    -Wno-uninitialized
76 .endif # WARNS >=2 && WARNS <= 4
77 CWARNFLAGS+=    -Wno-pointer-sign
78 # Clang has more warnings enabled by default, and when using -Wall, so if WARNS
79 # is set to low values, these have to be disabled explicitly.
80 .if ${WARNS} <= 6
81 CWARNFLAGS.clang+=      -Wno-empty-body -Wno-string-plus-int
82 CWARNFLAGS.clang+=      -Wno-unused-const-variable
83 .endif # WARNS <= 6
84 .if ${WARNS} <= 3
85 CWARNFLAGS.clang+=      -Wno-tautological-compare -Wno-unused-value\
86                 -Wno-parentheses-equality -Wno-unused-function -Wno-enum-conversion
87 CWARNFLAGS.clang+=      -Wno-unused-local-typedef
88 CWARNFLAGS.clang+=      -Wno-address-of-packed-member
89 .if ${COMPILER_TYPE} == "gcc" && ${COMPILER_VERSION} >= 90100
90 CWARNFLAGS.gcc+=        -Wno-address-of-packed-member
91 .endif
92 .if ${COMPILER_TYPE} == "clang" && ${COMPILER_VERSION} >= 70000 && \
93     ${MACHINE_CPUARCH} == "arm" && !${MACHINE_ARCH:Marmv[67]*}
94 CWARNFLAGS.clang+=      -Wno-atomic-alignment
95 .endif
96 .endif # WARNS <= 3
97 .if ${WARNS} <= 2
98 CWARNFLAGS.clang+=      -Wno-switch -Wno-switch-enum -Wno-knr-promoted-parameter
99 .endif # WARNS <= 2
100 .if ${WARNS} <= 1
101 CWARNFLAGS.clang+=      -Wno-parentheses
102 .endif # WARNS <= 1
103 .if defined(NO_WARRAY_BOUNDS)
104 CWARNFLAGS.clang+=      -Wno-array-bounds
105 .endif # NO_WARRAY_BOUNDS
106 .if defined(NO_WMISLEADING_INDENTATION) && \
107     ((${COMPILER_TYPE} == "clang" && ${COMPILER_VERSION} >= 100000) || \
108       ${COMPILER_TYPE} == "gcc")
109 CWARNFLAGS+=            -Wno-misleading-indentation
110 .endif # NO_WMISLEADING_INDENTATION
111 .endif # WARNS
112
113 .if defined(FORMAT_AUDIT)
114 WFORMAT=        1
115 .endif # FORMAT_AUDIT
116 .if defined(WFORMAT)
117 .if ${WFORMAT} > 0
118 #CWARNFLAGS+=   -Wformat-nonliteral -Wformat-security -Wno-format-extra-args
119 CWARNFLAGS+=    -Wformat=2 -Wno-format-extra-args
120 .if ${WARNS} <= 3
121 CWARNFLAGS.clang+=      -Wno-format-nonliteral
122 .endif # WARNS <= 3
123 .if ${MK_WERROR} != "no" && ${MK_WERROR.${COMPILER_TYPE}:Uyes} != "no"
124 CWARNFLAGS+=    -Werror
125 .endif # ${MK_WERROR} != "no" && ${MK_WERROR.${COMPILER_TYPE}:Uyes} != "no"
126 .endif # WFORMAT > 0
127 .endif # WFORMAT
128 .if defined(NO_WFORMAT) || defined(NO_WFORMAT.${COMPILER_TYPE})
129 CWARNFLAGS+=    -Wno-format
130 .endif # NO_WFORMAT || NO_WFORMAT.${COMPILER_TYPE}
131
132 # GCC
133 # We should clean up warnings produced with these flags.
134 # They were originally added as a quick hack to enable gcc5/6.
135 # The base system requires at least GCC 6.4, but some ports
136 # use this file with older compilers.  Request an exprun
137 # before changing these.
138 .if ${COMPILER_TYPE} == "gcc"
139 # GCC 5.2.0
140 .if ${COMPILER_VERSION} >= 50200
141 CWARNFLAGS+=    -Wno-error=address                      \
142                 -Wno-error=array-bounds                 \
143                 -Wno-error=attributes                   \
144                 -Wno-error=bool-compare                 \
145                 -Wno-error=cast-align                   \
146                 -Wno-error=clobbered                    \
147                 -Wno-error=deprecated-declarations      \
148                 -Wno-error=enum-compare                 \
149                 -Wno-error=extra                        \
150                 -Wno-error=logical-not-parentheses      \
151                 -Wno-error=strict-aliasing              \
152                 -Wno-error=uninitialized                \
153                 -Wno-error=unused-but-set-variable      \
154                 -Wno-error=unused-function              \
155                 -Wno-error=unused-value
156 .endif
157
158 # GCC 6.1.0
159 .if ${COMPILER_VERSION} >= 60100
160 CWARNFLAGS+=    -Wno-error=empty-body                   \
161                 -Wno-error=maybe-uninitialized          \
162                 -Wno-error=nonnull-compare              \
163                 -Wno-error=redundant-decls              \
164                 -Wno-error=shift-negative-value         \
165                 -Wno-error=tautological-compare         \
166                 -Wno-error=unused-const-variable
167 .endif
168
169 # GCC 7.1.0
170 .if ${COMPILER_VERSION} >= 70100
171 CWARNFLAGS+=    -Wno-error=bool-operation               \
172                 -Wno-error=deprecated                   \
173                 -Wno-error=expansion-to-defined         \
174                 -Wno-error=format-overflow              \
175                 -Wno-error=format-truncation            \
176                 -Wno-error=implicit-fallthrough         \
177                 -Wno-error=int-in-bool-context          \
178                 -Wno-error=memset-elt-size              \
179                 -Wno-error=noexcept-type                \
180                 -Wno-error=nonnull                      \
181                 -Wno-error=pointer-compare              \
182                 -Wno-error=stringop-overflow
183 .endif
184
185 # GCC 8.1.0
186 .if ${COMPILER_VERSION} >= 80100
187 CWARNFLAGS+=    -Wno-error=aggressive-loop-optimizations        \
188                 -Wno-error=cast-function-type                   \
189                 -Wno-error=catch-value                          \
190                 -Wno-error=multistatement-macros                \
191                 -Wno-error=restrict                             \
192                 -Wno-error=sizeof-pointer-memaccess             \
193                 -Wno-error=stringop-truncation
194 .endif
195
196 # GCC's own arm_neon.h triggers various warnings
197 .if ${MACHINE_CPUARCH} == "aarch64"
198 CWARNFLAGS+=    -Wno-system-headers
199 .endif
200 .endif  # gcc
201
202 # How to handle FreeBSD custom printf format specifiers.
203 .if ${COMPILER_TYPE} == "clang"
204 FORMAT_EXTENSIONS=      -D__printf__=__freebsd_kprintf__
205 .else
206 FORMAT_EXTENSIONS=      -fformat-extensions
207 .endif
208
209 .if defined(IGNORE_PRAGMA)
210 CWARNFLAGS+=    -Wno-unknown-pragmas
211 .endif # IGNORE_PRAGMA
212
213 # This warning is utter nonsense
214 CFLAGS+=        -Wno-format-zero-length
215
216 .if ${COMPILER_TYPE} == "clang"
217 # The headers provided by clang are incompatible with the FreeBSD headers.
218 # If the version of clang is not one that has been patched to omit the
219 # incompatible headers, we need to compile with -nobuiltininc and add the
220 # resource dir to the end of the search paths. This ensures that headers such as
221 # immintrin.h are still found but stddef.h, etc. are picked up from FreeBSD.
222 #
223 # XXX: This is a hack to support complete external installs of clang while
224 # we work to synchronize our decleration guards with those in the clang tree.
225 .if ${MK_CLANG_BOOTSTRAP:Uno} == "no" && \
226     ${COMPILER_RESOURCE_DIR} != "unknown" && !defined(BOOTSTRAPPING)
227 CFLAGS+=-nobuiltininc -idirafter ${COMPILER_RESOURCE_DIR}/include
228 .endif
229 .endif
230
231 CLANG_OPT_SMALL= -mstack-alignment=8 -mllvm -inline-threshold=3\
232                  -mllvm -simplifycfg-dup-ret
233 CLANG_OPT_SMALL+= -mllvm -enable-load-pre=false
234 CFLAGS.clang+=   -Qunused-arguments
235 # The libc++ headers use c++11 extensions.  These are normally silenced because
236 # they are treated as system headers, but we explicitly disable that warning
237 # suppression when building the base system to catch bugs in our headers.
238 # Eventually we'll want to start building the base system C++ code as C++11,
239 # but not yet.
240 CXXFLAGS.clang+=         -Wno-c++11-extensions
241
242 .if ${MK_SSP} != "no" && \
243     ${MACHINE_CPUARCH} != "arm" && ${MACHINE_CPUARCH} != "mips"
244 # Don't use -Wstack-protector as it breaks world with -Werror.
245 SSP_CFLAGS?=    -fstack-protector-strong
246 CFLAGS+=        ${SSP_CFLAGS}
247 .endif # SSP && !ARM && !MIPS
248
249 # Additional flags passed in CFLAGS and CXXFLAGS when MK_DEBUG_FILES is
250 # enabled.
251 DEBUG_FILES_CFLAGS?= -g
252
253 # Allow user-specified additional warning flags, plus compiler and file
254 # specific flag overrides, unless we've overridden this...
255 .if ${MK_WARNS} != "no"
256 CFLAGS+=        ${CWARNFLAGS:M*} ${CWARNFLAGS.${COMPILER_TYPE}}
257 CFLAGS+=        ${CWARNFLAGS.${.IMPSRC:T}}
258 CXXFLAGS+=      ${CXXWARNFLAGS:M*} ${CXXWARNFLAGS.${COMPILER_TYPE}}
259 CXXFLAGS+=      ${CXXWARNFLAGS.${.IMPSRC:T}}
260 .endif
261
262 CFLAGS+=         ${CFLAGS.${COMPILER_TYPE}}
263 CXXFLAGS+=       ${CXXFLAGS.${COMPILER_TYPE}}
264
265 AFLAGS+=        ${AFLAGS.${.IMPSRC:T}}
266 AFLAGS+=        ${AFLAGS.${.TARGET:T}}
267 ACFLAGS+=       ${ACFLAGS.${.IMPSRC:T}}
268 ACFLAGS+=       ${ACFLAGS.${.TARGET:T}}
269 CFLAGS+=        ${CFLAGS.${.IMPSRC:T}}
270 CXXFLAGS+=      ${CXXFLAGS.${.IMPSRC:T}}
271
272 LDFLAGS+=       ${LDFLAGS.${LINKER_TYPE}}
273
274 # Only allow .TARGET when not using PROGS as it has the same syntax
275 # per PROG which is ambiguous with this syntax. This is only needed
276 # for PROG_VARS vars.
277 .if !defined(_RECURSING_PROGS)
278 .if ${MK_WARNS} != "no"
279 CFLAGS+=        ${CWARNFLAGS.${.TARGET:T}}
280 .endif
281 CFLAGS+=        ${CFLAGS.${.TARGET:T}}
282 CXXFLAGS+=      ${CXXFLAGS.${.TARGET:T}}
283 LDFLAGS+=       ${LDFLAGS.${.TARGET:T}}
284 LDADD+=         ${LDADD.${.TARGET:T}}
285 LIBADD+=        ${LIBADD.${.TARGET:T}}
286 .endif
287
288 .if defined(SRCTOP)
289 # Prevent rebuilding during install to support read-only objdirs.
290 .if ${.TARGETS:M*install*} == ${.TARGETS} && empty(.MAKE.MODE:Mmeta)
291 CFLAGS+=        ERROR-tried-to-rebuild-during-make-install
292 .endif
293 .endif
294
295 # Please keep this if in sync with kern.mk
296 .if ${LD} != "ld" && (${CC:[1]:H} != ${LD:[1]:H} || ${LD:[1]:T} != "ld")
297 # Add -fuse-ld=${LD} if $LD is in a different directory or not called "ld".
298 .if ${COMPILER_TYPE} == "clang"
299 # Note: Clang does not like relative paths for ld so we map ld.lld -> lld.
300 .if ${COMPILER_VERSION} >= 120000
301 LDFLAGS+=       --ld-path=${LD:[1]:S/^ld.//1W}
302 .else
303 LDFLAGS+=       -fuse-ld=${LD:[1]:S/^ld.//1W}
304 .endif
305 .else
306 # GCC does not support an absolute path for -fuse-ld so we just print this
307 # warning instead and let the user add the required symlinks.
308 # However, we can avoid this warning if -B is set appropriately (e.g. for
309 # CROSS_TOOLCHAIN=...-gcc).
310 .if !(${LD:[1]:T} == "ld" && ${CC:tw:M-B${LD:[1]:H}/})
311 .warning LD (${LD}) is not the default linker for ${CC} but -fuse-ld= is not supported
312 .endif
313 .endif
314 .endif
315
316 # Tell bmake not to mistake standard targets for things to be searched for
317 # or expect to ever be up-to-date.
318 PHONY_NOTMAIN = analyze afterdepend afterinstall all beforedepend beforeinstall \
319                 beforelinking build build-tools buildconfig buildfiles \
320                 buildincludes check checkdpadd clean cleandepend cleandir \
321                 cleanobj configure depend distclean distribute exe \
322                 files html includes install installconfig installdirs \
323                 installfiles installincludes lint obj objlink objs objwarn \
324                 realinstall tags whereobj
325
326 # we don't want ${PROG} to be PHONY
327 .PHONY: ${PHONY_NOTMAIN:N${PROG:U}}
328 .NOTMAIN: ${PHONY_NOTMAIN:Nall}
329
330 .if ${MK_STAGING} != "no"
331 .if defined(_SKIP_BUILD) || (!make(all) && !make(clean*) && !make(*clean))
332 _SKIP_STAGING?= yes
333 .endif
334 .if ${_SKIP_STAGING:Uno} == "yes"
335 staging stage_libs stage_files stage_as stage_links stage_symlinks:
336 .else
337 # allow targets like beforeinstall to be leveraged
338 DESTDIR= ${STAGE_OBJTOP}
339 .export DESTDIR
340
341 .if target(beforeinstall)
342 .if !empty(_LIBS) || (${MK_STAGING_PROG} != "no" && !defined(INTERNALPROG))
343 staging: beforeinstall
344 .endif
345 .endif
346
347 # normally only libs and includes are staged
348 .if ${MK_STAGING_PROG} != "no" && !defined(INTERNALPROG)
349 STAGE_DIR.prog= ${STAGE_OBJTOP}${BINDIR}
350
351 .if !empty(PROG)
352 .if defined(PROGNAME)
353 STAGE_AS_SETS+= prog
354 STAGE_AS_${PROG}= ${PROGNAME}
355 stage_as.prog: ${PROG}
356 .else
357 STAGE_SETS+= prog
358 stage_files.prog: ${PROG}
359 STAGE_TARGETS+= stage_files
360 .endif
361 .endif
362 .endif
363
364 .if !empty(_LIBS) && !defined(INTERNALLIB)
365 .if defined(SHLIBDIR) && ${SHLIBDIR} != ${LIBDIR} && ${_LIBS:Uno:M*.so.*} != ""
366 STAGE_SETS+= shlib
367 STAGE_DIR.shlib= ${STAGE_OBJTOP}${SHLIBDIR}
368 STAGE_FILES.shlib+= ${_LIBS:M*.so.*}
369 stage_files.shlib: ${_LIBS:M*.so.*}
370 .endif
371
372 .if defined(SHLIB_LINK) && commands(${SHLIB_LINK:R}.ld)
373 STAGE_AS_SETS+= ldscript
374 STAGE_AS.ldscript+= ${SHLIB_LINK:R}.ld
375 stage_as.ldscript: ${SHLIB_LINK:R}.ld
376 STAGE_DIR.ldscript = ${STAGE_LIBDIR}
377 STAGE_AS_${SHLIB_LINK:R}.ld:= ${SHLIB_LINK}
378 NO_SHLIB_LINKS=
379 .endif
380
381 .if target(stage_files.shlib)
382 stage_libs: ${_LIBS}
383 .if defined(DEBUG_FLAGS) && target(${SHLIB_NAME}.symbols)
384 stage_files.shlib: ${SHLIB_NAME}.symbols
385 .endif
386 .else
387 stage_libs: ${_LIBS}
388 .endif
389 .if defined(SHLIB_NAME) && defined(DEBUG_FLAGS) && target(${SHLIB_NAME}.symbols)
390 stage_libs: ${SHLIB_NAME}.symbols
391 .endif
392
393 .endif
394
395 .if !empty(INCS) || !empty(INCSGROUPS) && target(buildincludes)
396 .if !defined(NO_BEFOREBUILD_INCLUDES)
397 stage_includes: buildincludes
398 beforebuild: stage_includes
399 .endif
400 .endif
401
402 .for t in stage_libs stage_files stage_as
403 .if target($t)
404 STAGE_TARGETS+= $t
405 .endif
406 .endfor
407
408 .if !empty(STAGE_AS_SETS)
409 STAGE_TARGETS+= stage_as
410 .endif
411
412 .if !empty(STAGE_TARGETS) || (${MK_STAGING_PROG} != "no" && !defined(INTERNALPROG))
413
414 .if !empty(LINKS)
415 STAGE_TARGETS+= stage_links
416 .if ${MAKE_VERSION} < 20131001
417 stage_links.links: ${_LIBS} ${PROG}
418 .endif
419 STAGE_SETS+= links
420 STAGE_LINKS.links= ${LINKS}
421 .endif
422
423 .if !empty(SYMLINKS)
424 STAGE_TARGETS+= stage_symlinks
425 STAGE_SETS+= links
426 STAGE_SYMLINKS.links= ${SYMLINKS}
427 .endif
428
429 .endif
430
431 .include <meta.stage.mk>
432 .endif
433 .endif
434
435 .if defined(META_TARGETS)
436 .for _tgt in ${META_TARGETS}
437 .if target(${_tgt})
438 ${_tgt}: ${META_DEPS}
439 .endif
440 .endfor
441 .endif