1 # 1 #
2 # arch/arm64/Makefile !! 2 # alpha/Makefile
3 # <<
4 # This file is included by the global makefile <<
5 # architecture-specific flags and dependencies <<
6 # 3 #
7 # This file is subject to the terms and condit 4 # This file is subject to the terms and conditions of the GNU General Public
8 # License. See the file "COPYING" in the main 5 # License. See the file "COPYING" in the main directory of this archive
9 # for more details. 6 # for more details.
10 # 7 #
11 # Copyright (C) 1995-2001 by Russell King !! 8 # Copyright (C) 1994 by Linus Torvalds
>> 9 #
12 10
13 LDFLAGS_vmlinux :=--no-undefined -X --pic-vene !! 11 NM := $(NM) -B
14 12
15 ifeq ($(CONFIG_RELOCATABLE), y) !! 13 LDFLAGS_vmlinux := -static -N #-relax
16 # Pass --no-apply-dynamic-relocs to restore pr !! 14 CHECKFLAGS += -D__alpha__
17 # for relative relocs, since this leads to bet !! 15 cflags-y := -pipe -mno-fp-regs -ffixed-8
18 # with the relocation offsets always being zer !! 16 cflags-y += $(call cc-option, -fno-jump-tables)
19 LDFLAGS_vmlinux += -shared -Bsymbolic <<
20 $(call ld-option, --no <<
21 endif <<
22 <<
23 ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) <<
24 ifeq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_8434 <<
25 LDFLAGS_vmlinux += --fix-cortex-a53-843419 <<
26 endif <<
27 endif <<
28 <<
29 cc_has_k_constraint := $(call try-run,echo <<
30 'int main(void) { <<
31 asm volatile("and w0, w0, %w0" <<
32 return 0; <<
33 }' | $(CC) -S -x c -o "$$TMP" -,,-DCON <<
34 <<
35 ifeq ($(CONFIG_BROKEN_GAS_INST),y) <<
36 $(warning Detected assembler with broken .inst <<
37 endif <<
38 <<
39 # The GCC option -ffreestanding is required in <<
40 # ARM/NEON intrinsics in a non C99-compliant e <<
41 CC_FLAGS_FPU := -ffreestanding <<
42 # Enable <arm_neon.h> <<
43 CC_FLAGS_FPU += -isystem $(shell $(CC) -pri <<
44 CC_FLAGS_NO_FPU := -mgeneral-regs-only <<
45 <<
46 KBUILD_CFLAGS += $(CC_FLAGS_NO_FPU) \ <<
47 $(compat_vdso) $(cc_has_k_c <<
48 KBUILD_CFLAGS += $(call cc-disable-warning, <<
49 KBUILD_AFLAGS += $(compat_vdso) <<
50 <<
51 KBUILD_RUSTFLAGS += --target=aarch64-unknown-n <<
52 <<
53 KBUILD_CFLAGS += $(call cc-option,-mabi=lp64 <<
54 KBUILD_AFLAGS += $(call cc-option,-mabi=lp64 <<
55 <<
56 # Avoid generating .eh_frame* sections. <<
57 ifneq ($(CONFIG_UNWIND_TABLES),y) <<
58 KBUILD_CFLAGS += -fno-asynchronous-unwind-ta <<
59 KBUILD_AFLAGS += -fno-asynchronous-unwind-ta <<
60 KBUILD_RUSTFLAGS += -Cforce-unwind-tables=n <<
61 else <<
62 KBUILD_CFLAGS += -fasynchronous-unwind-table <<
63 KBUILD_AFLAGS += -fasynchronous-unwind-table <<
64 KBUILD_RUSTFLAGS += -Cforce-unwind-tables=y -Z <<
65 endif <<
66 <<
67 ifeq ($(CONFIG_STACKPROTECTOR_PER_TASK),y) <<
68 prepare: stack_protector_prepare <<
69 stack_protector_prepare: prepare0 <<
70 $(eval KBUILD_CFLAGS += -mstack-protec <<
71 -mstack-protec <<
72 -mstack-protec <<
73 awk '{if ($$2 == "TSK_ <<
74 includ <<
75 endif <<
76 <<
77 ifeq ($(CONFIG_ARM64_BTI_KERNEL),y) <<
78 KBUILD_CFLAGS += -mbranch-protection=pac-ret <<
79 KBUILD_RUSTFLAGS += -Zbranch-protection=bti, <<
80 else ifeq ($(CONFIG_ARM64_PTR_AUTH_KERNEL),y) <<
81 KBUILD_RUSTFLAGS += -Zbranch-protection=pac- <<
82 ifeq ($(CONFIG_CC_HAS_BRANCH_PROT_PAC_RET),y <<
83 KBUILD_CFLAGS += -mbranch-protection=pac-r <<
84 else <<
85 KBUILD_CFLAGS += -msign-return-address=non <<
86 endif <<
87 else <<
88 KBUILD_CFLAGS += $(call cc-option,-mbranch-p <<
89 endif <<
90 17
91 # Tell the assembler to support instructions f !! 18 cpuflags-$(CONFIG_ALPHA_EV56) := -mcpu=ev56
92 # architecture. !! 19 cpuflags-$(CONFIG_ALPHA_POLARIS) := -mcpu=pca56
93 # !! 20 cpuflags-$(CONFIG_ALPHA_SX164) := -mcpu=pca56
94 # For non-integrated assemblers we'll pass thi !! 21 cpuflags-$(CONFIG_ALPHA_EV6) := -mcpu=ev6
95 # integrated assemblers we'll define ARM64_ASM !! 22 cpuflags-$(CONFIG_ALPHA_EV67) := -mcpu=ev67
96 # inline usage. !! 23 # If GENERIC, make sure to turn off any instruction set extensions that
97 # !! 24 # the host compiler might have on by default.
98 # We cannot pass the same arch flag to the com !! 25 cpuflags-$(CONFIG_ALPHA_GENERIC) := -mcpu=ev56 -mtune=ev6
99 # freely generate instructions which are not s <<
100 # versions, which would prevent a single kerne <<
101 # hardware. <<
102 ifeq ($(CONFIG_AS_HAS_ARMV8_5), y) <<
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 <<
110 endif <<
111 <<
112 ifdef asm-arch <<
113 KBUILD_CFLAGS += -Wa,-march=$(asm-arch) \ <<
114 -DARM64_ASM_ARCH='"$(asm-ar <<
115 endif <<
116 <<
117 ifeq ($(CONFIG_SHADOW_CALL_STACK), y) <<
118 KBUILD_CFLAGS += -ffixed-x18 <<
119 KBUILD_RUSTFLAGS += -Zfixed-x18 <<
120 endif <<
121 <<
122 ifeq ($(CONFIG_CPU_BIG_ENDIAN), y) <<
123 KBUILD_CPPFLAGS += -mbig-endian <<
124 CHECKFLAGS += -D__AARCH64EB__ <<
125 # Prefer the baremetal ELF build target, but n <<
126 # it so fall back to the standard linux versio <<
127 KBUILD_LDFLAGS += -EB $(call ld-option, -maar <<
128 UTS_MACHINE := aarch64_be <<
129 else <<
130 KBUILD_CPPFLAGS += -mlittle-endian <<
131 CHECKFLAGS += -D__AARCH64EL__ <<
132 # Same as above, prefer ELF but fall back to l <<
133 KBUILD_LDFLAGS += -EL $(call ld-option, -maar <<
134 UTS_MACHINE := aarch64 <<
135 endif <<
136 <<
137 ifeq ($(CONFIG_LD_IS_LLD), y) <<
138 KBUILD_LDFLAGS += -z norelro <<
139 endif <<
140 <<
141 CHECKFLAGS += -D__aarch64__ <<
142 <<
143 ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_CALL_OPS),y <<
144 KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNC <<
145 CC_FLAGS_FTRACE := -fpatchable-function-entr <<
146 else ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_ARGS), <<
147 KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNC <<
148 CC_FLAGS_FTRACE := -fpatchable-function-entr <<
149 endif <<
150 <<
151 ifeq ($(CONFIG_KASAN_SW_TAGS), y) <<
152 KASAN_SHADOW_SCALE_SHIFT := 4 <<
153 else ifeq ($(CONFIG_KASAN_GENERIC), y) <<
154 KASAN_SHADOW_SCALE_SHIFT := 3 <<
155 endif <<
156 <<
157 KBUILD_CFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$( <<
158 KBUILD_CPPFLAGS += -DKASAN_SHADOW_SCALE_SHIFT= <<
159 KBUILD_AFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$( <<
160 <<
161 libs-y := arch/arm64/lib/ $(libs-y) <<
162 libs-$(CONFIG_EFI_STUB) += $(objtree)/drivers/ <<
163 <<
164 # Default target when executing plain make <<
165 boot := arch/arm64/boot <<
166 <<
167 BOOT_TARGETS := Image vmlinuz.efi image.fit <<
168 <<
169 PHONY += $(BOOT_TARGETS) <<
170 <<
171 ifeq ($(CONFIG_EFI_ZBOOT),) <<
172 KBUILD_IMAGE := $(boot)/Image.gz <<
173 else <<
174 KBUILD_IMAGE := $(boot)/vmlinuz.efi <<
175 endif <<
176 26
177 all: $(notdir $(KBUILD_IMAGE)) !! 27 cflags-y += $(cpuflags-y)
178 28
179 image.fit: dtbs <<
180 29
181 vmlinuz.efi image.fit: Image !! 30 # For TSUNAMI, we must have the assembler not emulate our instructions.
182 $(BOOT_TARGETS): vmlinux !! 31 # The same is true for IRONGATE, POLARIS, PYXIS.
183 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ !! 32 # BWX is most important, but we don't really want any emulation ever.
>> 33 KBUILD_CFLAGS += $(cflags-y) -Wa,-mev6
>> 34
>> 35 libs-y += arch/alpha/lib/
>> 36
>> 37 # export what is needed by arch/alpha/boot/Makefile
>> 38 LIBS_Y := $(patsubst %/, %/lib.a, $(libs-y))
>> 39 export LIBS_Y
>> 40
>> 41 boot := arch/alpha/boot
>> 42
>> 43 #Default target when executing make with no arguments
>> 44 all boot: $(boot)/vmlinux.gz
>> 45
>> 46 $(boot)/vmlinux.gz: vmlinux
>> 47 $(Q)$(MAKE) $(build)=$(boot) $@
184 48
185 Image.%: Image !! 49 bootimage bootpfile bootpzfile: vmlinux
186 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ 50 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$@
187 51
188 ifeq ($(CONFIG_COMPRESSED_INSTALL),y) !! 52 archheaders:
189 DEFAULT_KBUILD_IMAGE = $(KBUILD_IMAGE) !! 53 $(Q)$(MAKE) $(build)=arch/alpha/kernel/syscalls all
190 else <<
191 DEFAULT_KBUILD_IMAGE = $(boot)/Image <<
192 endif <<
193 <<
194 install: KBUILD_IMAGE := $(DEFAULT_KBUILD_IMAG <<
195 install zinstall: <<
196 $(call cmd,install) <<
197 <<
198 archprepare: <<
199 $(Q)$(MAKE) $(build)=arch/arm64/tools <<
200 ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) <<
201 ifneq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_843 <<
202 @echo "warning: ld does not support -- <<
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 suppor <<
208 endif <<
209 endif <<
210 <<
211 ifeq ($(KBUILD_EXTMOD),) <<
212 # We need to generate vdso-offsets.h before co <<
213 # In order to do that, we should use the archp <<
214 # asm-offsets.h is included in some files used <<
215 # asm-offsets.h is built in prepare0, for whic <<
216 # Therefore we need to generate the header aft <<
217 # this hack. <<
218 prepare: vdso_prepare <<
219 vdso_prepare: prepare0 <<
220 $(Q)$(MAKE) $(build)=arch/arm64/kernel <<
221 include/generated/vdso-offsets.h arch/ <<
222 ifdef CONFIG_COMPAT_VDSO <<
223 $(Q)$(MAKE) $(build)=arch/arm64/kernel <<
224 arch/arm64/kernel/vdso32/vdso.so <<
225 endif <<
226 endif <<
227 <<
228 vdso-install-y += arc <<
229 vdso-install-$(CONFIG_COMPAT_VDSO) += arc <<
230 <<
231 include $(srctree)/scripts/Makefile.defconf <<
232 <<
233 PHONY += virtconfig <<
234 virtconfig: <<
235 $(call merge_into_defconfig_override,d <<
236 54
237 define archhelp 55 define archhelp
238 echo '* Image.gz - Compressed kernel i !! 56 echo '* boot - Compressed kernel image (arch/alpha/boot/vmlinux.gz)'
239 echo ' Image - Uncompressed kernel !! 57 echo ' bootimage - SRM bootable image (arch/alpha/boot/bootimage)'
240 echo ' image.fit - Flat Image Tree (ar !! 58 echo ' bootpfile - BOOTP bootable image (arch/alpha/boot/bootpfile)'
241 echo ' install - Install kernel (com !! 59 echo ' bootpzfile - compressed kernel BOOTP image (arch/alpha/boot/bootpzfile)'
242 echo ' zinstall - Install compressed <<
243 echo ' Install using (your <<
244 echo ' (distribution) /sbi <<
245 echo ' install to $$(INSTA <<
246 endef 60 endef
Linux® is a registered trademark of Linus Torvalds in the United States and other countries.
TOMOYO® is a registered trademark of NTT DATA CORPORATION.