Commit | Line | Data |
---|---|---|
8c2c3df3 CM |
1 | # |
2 | # arch/arm64/Makefile | |
3 | # | |
4 | # This file is included by the global makefile so that you can add your own | |
5 | # architecture-specific flags and dependencies. | |
6 | # | |
7 | # This file is subject to the terms and conditions of the GNU General Public | |
8 | # License. See the file "COPYING" in the main directory of this archive | |
9 | # for more details. | |
10 | # | |
11 | # Copyright (C) 1995-2001 by Russell King | |
12 | ||
311bea3c | 13 | LDFLAGS_vmlinux :=--no-undefined -X |
8c2c3df3 | 14 | |
fd9dde6a ND |
15 | ifeq ($(CONFIG_RELOCATABLE), y) |
16 | # Pass --no-apply-dynamic-relocs to restore pre-binutils-2.27 behaviour | |
17 | # for relative relocs, since this leads to better Image compression | |
18 | # with the relocation offsets always being zero. | |
3b92fa74 | 19 | LDFLAGS_vmlinux += -shared -Bsymbolic -z notext \ |
fd9dde6a | 20 | $(call ld-option, --no-apply-dynamic-relocs) |
1e48ef7f AB |
21 | endif |
22 | ||
6ffe9923 | 23 | ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) |
64ee84c7 | 24 | ifeq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_843419),y) |
6ffe9923 WD |
25 | LDFLAGS_vmlinux += --fix-cortex-a53-843419 |
26 | endif | |
27 | endif | |
28 | ||
03adcbd9 WD |
29 | cc_has_k_constraint := $(call try-run,echo \ |
30 | 'int main(void) { \ | |
31 | asm volatile("and w0, w0, %w0" :: "K" (4294967295)); \ | |
32 | return 0; \ | |
33 | }' | $(CC) -S -x c -o "$$TMP" -,,-DCONFIG_CC_HAS_K_CONSTRAINT=1) | |
34 | ||
8bf9284d | 35 | ifeq ($(CONFIG_BROKEN_GAS_INST),y) |
bbb56c27 MZ |
36 | $(warning Detected assembler with broken .inst; disassembly will be unreliable) |
37 | endif | |
38 | ||
71883ae3 SH |
39 | # The GCC option -ffreestanding is required in order to compile code containing |
40 | # ARM/NEON intrinsics in a non C99-compliant environment (such as the kernel) | |
41 | CC_FLAGS_FPU := -ffreestanding | |
42 | # Enable <arm_neon.h> | |
43 | CC_FLAGS_FPU += -isystem $(shell $(CC) -print-file-name=include) | |
44 | CC_FLAGS_NO_FPU := -mgeneral-regs-only | |
45 | ||
46 | KBUILD_CFLAGS += $(CC_FLAGS_NO_FPU) \ | |
03adcbd9 | 47 | $(compat_vdso) $(cc_has_k_constraint) |
fa63da2a | 48 | KBUILD_CFLAGS += $(call cc-disable-warning, psabi) |
8bf9284d | 49 | KBUILD_AFLAGS += $(compat_vdso) |
c09d6a04 | 50 | |
724a75ac JC |
51 | KBUILD_RUSTFLAGS += --target=aarch64-unknown-none -Ctarget-feature="-neon" |
52 | ||
3d6a7b99 AP |
53 | KBUILD_CFLAGS += $(call cc-option,-mabi=lp64) |
54 | KBUILD_AFLAGS += $(call cc-option,-mabi=lp64) | |
55 | ||
6e0a66d1 | 56 | # Avoid generating .eh_frame* sections. |
68c76ad4 | 57 | ifneq ($(CONFIG_UNWIND_TABLES),y) |
6e0a66d1 KC |
58 | KBUILD_CFLAGS += -fno-asynchronous-unwind-tables -fno-unwind-tables |
59 | KBUILD_AFLAGS += -fno-asynchronous-unwind-tables -fno-unwind-tables | |
d077242d | 60 | KBUILD_RUSTFLAGS += -Cforce-unwind-tables=n |
68c76ad4 AB |
61 | else |
62 | KBUILD_CFLAGS += -fasynchronous-unwind-tables | |
63 | KBUILD_AFLAGS += -fasynchronous-unwind-tables | |
d077242d | 64 | KBUILD_RUSTFLAGS += -Cforce-unwind-tables=y -Zuse-sync-unwind=n |
68c76ad4 | 65 | endif |
6e0a66d1 | 66 | |
0a1213fa AB |
67 | ifeq ($(CONFIG_STACKPROTECTOR_PER_TASK),y) |
68 | prepare: stack_protector_prepare | |
69 | stack_protector_prepare: prepare0 | |
70 | $(eval KBUILD_CFLAGS += -mstack-protector-guard=sysreg \ | |
71 | -mstack-protector-guard-reg=sp_el0 \ | |
72 | -mstack-protector-guard-offset=$(shell \ | |
73 | awk '{if ($$2 == "TSK_STACK_CANARY") print $$3;}' \ | |
74 | include/generated/asm-offsets.h)) | |
75 | endif | |
76 | ||
92e2294d | 77 | ifeq ($(CONFIG_ARM64_BTI_KERNEL),y) |
c68cf528 | 78 | KBUILD_CFLAGS += -mbranch-protection=pac-ret+bti |
724a75ac | 79 | KBUILD_RUSTFLAGS += -Zbranch-protection=bti,pac-ret |
c68cf528 | 80 | else ifeq ($(CONFIG_ARM64_PTR_AUTH_KERNEL),y) |
724a75ac | 81 | KBUILD_RUSTFLAGS += -Zbranch-protection=pac-ret |
c68cf528 MR |
82 | ifeq ($(CONFIG_CC_HAS_BRANCH_PROT_PAC_RET),y) |
83 | KBUILD_CFLAGS += -mbranch-protection=pac-ret | |
84 | else | |
85 | KBUILD_CFLAGS += -msign-return-address=non-leaf | |
86 | endif | |
92e2294d | 87 | else |
c68cf528 | 88 | KBUILD_CFLAGS += $(call cc-option,-mbranch-protection=none) |
1764c3ed ST |
89 | endif |
90 | ||
1e249c41 MR |
91 | # Tell the assembler to support instructions from the latest target |
92 | # architecture. | |
93 | # | |
94 | # For non-integrated assemblers we'll pass this on the command line, and for | |
95 | # integrated assemblers we'll define ARM64_ASM_ARCH and ARM64_ASM_PREAMBLE for | |
96 | # inline usage. | |
97 | # | |
98 | # We cannot pass the same arch flag to the compiler as this would allow it to | |
99 | # freely generate instructions which are not supported by earlier architecture | |
100 | # versions, which would prevent a single kernel image from working on earlier | |
101 | # hardware. | |
f469c032 | 102 | ifeq ($(CONFIG_AS_HAS_ARMV8_5), y) |
1e249c41 MR |
103 | asm-arch := armv8.5-a |
104 | else ifeq ($(CONFIG_AS_HAS_ARMV8_4), y) | |
105 | asm-arch := armv8.4-a | |
106 | else ifeq ($(CONFIG_AS_HAS_ARMV8_3), y) | |
107 | asm-arch := armv8.3-a | |
108 | else ifeq ($(CONFIG_AS_HAS_ARMV8_2), y) | |
109 | asm-arch := armv8.2-a | |
f469c032 VF |
110 | endif |
111 | ||
1764c3ed ST |
112 | ifdef asm-arch |
113 | KBUILD_CFLAGS += -Wa,-march=$(asm-arch) \ | |
114 | -DARM64_ASM_ARCH='"$(asm-arch)"' | |
7c78f67e ZY |
115 | endif |
116 | ||
da64e9d1 ST |
117 | ifeq ($(CONFIG_SHADOW_CALL_STACK), y) |
118 | KBUILD_CFLAGS += -ffixed-x18 | |
d077242d | 119 | KBUILD_RUSTFLAGS += -Zfixed-x18 |
da64e9d1 ST |
120 | endif |
121 | ||
a0974e6e WD |
122 | ifeq ($(CONFIG_CPU_BIG_ENDIAN), y) |
123 | KBUILD_CPPFLAGS += -mbig-endian | |
bcde519e | 124 | CHECKFLAGS += -D__AARCH64EB__ |
c931d34e OJ |
125 | # Prefer the baremetal ELF build target, but not all toolchains include |
126 | # it so fall back to the standard linux version if needed. | |
311bea3c | 127 | KBUILD_LDFLAGS += -EB $(call ld-option, -maarch64elfb, -maarch64linuxb -z norelro) |
cfa88c79 | 128 | UTS_MACHINE := aarch64_be |
a0974e6e | 129 | else |
8c2c3df3 | 130 | KBUILD_CPPFLAGS += -mlittle-endian |
bcde519e | 131 | CHECKFLAGS += -D__AARCH64EL__ |
c931d34e | 132 | # Same as above, prefer ELF but fall back to linux target if needed. |
311bea3c | 133 | KBUILD_LDFLAGS += -EL $(call ld-option, -maarch64elf, -maarch64linux -z norelro) |
cfa88c79 | 134 | UTS_MACHINE := aarch64 |
a0974e6e | 135 | endif |
8c2c3df3 | 136 | |
311bea3c ND |
137 | ifeq ($(CONFIG_LD_IS_LLD), y) |
138 | KBUILD_LDFLAGS += -z norelro | |
139 | endif | |
140 | ||
1f2f01b1 | 141 | CHECKFLAGS += -D__aarch64__ |
8c2c3df3 | 142 | |
baaf553d MR |
143 | ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_CALL_OPS),y) |
144 | KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNCTION_ENTRY | |
145 | CC_FLAGS_FTRACE := -fpatchable-function-entry=4,2 | |
146 | else ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_ARGS),y) | |
3b23e499 TD |
147 | KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNCTION_ENTRY |
148 | CC_FLAGS_FTRACE := -fpatchable-function-entry=2 | |
149 | endif | |
150 | ||
b2f557ea AK |
151 | ifeq ($(CONFIG_KASAN_SW_TAGS), y) |
152 | KASAN_SHADOW_SCALE_SHIFT := 4 | |
0fea6e9a | 153 | else ifeq ($(CONFIG_KASAN_GENERIC), y) |
b2f557ea AK |
154 | KASAN_SHADOW_SCALE_SHIFT := 3 |
155 | endif | |
156 | ||
157 | KBUILD_CFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$(KASAN_SHADOW_SCALE_SHIFT) | |
158 | KBUILD_CPPFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$(KASAN_SHADOW_SCALE_SHIFT) | |
159 | KBUILD_AFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$(KASAN_SHADOW_SCALE_SHIFT) | |
160 | ||
8c2c3df3 | 161 | libs-y := arch/arm64/lib/ $(libs-y) |
c1aac64d | 162 | libs-$(CONFIG_EFI_STUB) += $(objtree)/drivers/firmware/efi/libstub/lib.a |
8c2c3df3 CM |
163 | |
164 | # Default target when executing plain make | |
06995804 | 165 | boot := arch/arm64/boot |
c37b830f | 166 | |
7a23b027 | 167 | BOOT_TARGETS := Image vmlinuz.efi image.fit |
0dc1670b SG |
168 | |
169 | PHONY += $(BOOT_TARGETS) | |
170 | ||
c37b830f | 171 | ifeq ($(CONFIG_EFI_ZBOOT),) |
06995804 | 172 | KBUILD_IMAGE := $(boot)/Image.gz |
c37b830f AB |
173 | else |
174 | KBUILD_IMAGE := $(boot)/vmlinuz.efi | |
175 | endif | |
8c2c3df3 | 176 | |
c37b830f | 177 | all: $(notdir $(KBUILD_IMAGE)) |
8c2c3df3 | 178 | |
7a23b027 SG |
179 | image.fit: dtbs |
180 | ||
181 | vmlinuz.efi image.fit: Image | |
0dc1670b | 182 | $(BOOT_TARGETS): vmlinux |
0723c05f OJ |
183 | $(Q)$(MAKE) $(build)=$(boot) $(boot)/$@ |
184 | ||
9ca4e58c | 185 | Image.%: Image |
70f915a2 | 186 | $(Q)$(MAKE) $(build)=$(boot) $(boot)/$@ |
8c2c3df3 | 187 | |
4c7be57f LT |
188 | ifeq ($(CONFIG_COMPRESSED_INSTALL),y) |
189 | DEFAULT_KBUILD_IMAGE = $(KBUILD_IMAGE) | |
190 | else | |
191 | DEFAULT_KBUILD_IMAGE = $(boot)/Image | |
192 | endif | |
193 | ||
194 | install: KBUILD_IMAGE := $(DEFAULT_KBUILD_IMAGE) | |
70a4039b | 195 | install zinstall: |
f774f5bb | 196 | $(call cmd,install) |
8c2c3df3 | 197 | |
0c6c2d36 MB |
198 | archprepare: |
199 | $(Q)$(MAKE) $(build)=arch/arm64/tools kapi | |
64ee84c7 MY |
200 | ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) |
201 | ifneq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_843419),y) | |
202 | @echo "warning: ld does not support --fix-cortex-a53-843419; kernel may be susceptible to erratum" >&2 | |
203 | endif | |
204 | endif | |
205 | ifeq ($(CONFIG_ARM64_USE_LSE_ATOMICS),y) | |
206 | ifneq ($(CONFIG_ARM64_LSE_ATOMICS),y) | |
207 | @echo "warning: LSE atomics not supported by binutils" >&2 | |
208 | endif | |
209 | endif | |
210 | ||
98356eb0 | 211 | ifeq ($(KBUILD_EXTMOD),) |
a66649da KB |
212 | # We need to generate vdso-offsets.h before compiling certain files in kernel/. |
213 | # In order to do that, we should use the archprepare target, but we can't since | |
214 | # asm-offsets.h is included in some files used to generate vdso-offsets.h, and | |
215 | # asm-offsets.h is built in prepare0, for which archprepare is a dependency. | |
216 | # Therefore we need to generate the header after prepare0 has been made, hence | |
217 | # this hack. | |
218 | prepare: vdso_prepare | |
219 | vdso_prepare: prepare0 | |
a5b8ca97 MY |
220 | $(Q)$(MAKE) $(build)=arch/arm64/kernel/vdso \ |
221 | include/generated/vdso-offsets.h arch/arm64/kernel/vdso/vdso.so | |
222 | ifdef CONFIG_COMPAT_VDSO | |
223 | $(Q)$(MAKE) $(build)=arch/arm64/kernel/vdso32 \ | |
c7767f5c | 224 | arch/arm64/kernel/vdso32/vdso.so |
a5b8ca97 | 225 | endif |
98356eb0 | 226 | endif |
a66649da | 227 | |
56769ba4 | 228 | vdso-install-y += arch/arm64/kernel/vdso/vdso.so.dbg |
a099bec7 | 229 | vdso-install-$(CONFIG_COMPAT_VDSO) += arch/arm64/kernel/vdso32/vdso32.so.dbg |
56769ba4 | 230 | |
c6cd63f5 MB |
231 | include $(srctree)/scripts/Makefile.defconf |
232 | ||
233 | PHONY += virtconfig | |
234 | virtconfig: | |
235 | $(call merge_into_defconfig_override,defconfig,virt) | |
236 | ||
8c2c3df3 CM |
237 | define archhelp |
238 | echo '* Image.gz - Compressed kernel image (arch/$(ARCH)/boot/Image.gz)' | |
239 | echo ' Image - Uncompressed kernel image (arch/$(ARCH)/boot/Image)' | |
7a23b027 | 240 | echo ' image.fit - Flat Image Tree (arch/$(ARCH)/boot/image.fit)' |
4c7be57f | 241 | echo ' install - Install kernel (compressed if COMPRESSED_INSTALL set)' |
8c2c3df3 CM |
242 | echo ' zinstall - Install compressed kernel' |
243 | echo ' Install using (your) ~/bin/installkernel or' | |
244 | echo ' (distribution) /sbin/installkernel or' | |
245 | echo ' install to $$(INSTALL_PATH) and run lilo' | |
246 | endef |