Linux/arch/arm64/Makefile

Version: ~ [ linux-6.12-rc7 ] ~ [ linux-6.11.7 ] ~ [ linux-6.10.14 ] ~ [ linux-6.9.12 ] ~ [ linux-6.8.12 ] ~ [ linux-6.7.12 ] ~ [ linux-6.6.60 ] ~ [ linux-6.5.13 ] ~ [ linux-6.4.16 ] ~ [ linux-6.3.13 ] ~ [ linux-6.2.16 ] ~ [ linux-6.1.116 ] ~ [ linux-6.0.19 ] ~ [ linux-5.19.17 ] ~ [ linux-5.18.19 ] ~ [ linux-5.17.15 ] ~ [ linux-5.16.20 ] ~ [ linux-5.15.171 ] ~ [ linux-5.14.21 ] ~ [ linux-5.13.19 ] ~ [ linux-5.12.19 ] ~ [ linux-5.11.22 ] ~ [ linux-5.10.229 ] ~ [ linux-5.9.16 ] ~ [ linux-5.8.18 ] ~ [ linux-5.7.19 ] ~ [ linux-5.6.19 ] ~ [ linux-5.5.19 ] ~ [ linux-5.4.285 ] ~ [ linux-5.3.18 ] ~ [ linux-5.2.21 ] ~ [ linux-5.1.21 ] ~ [ linux-5.0.21 ] ~ [ linux-4.20.17 ] ~ [ linux-4.19.323 ] ~ [ linux-4.18.20 ] ~ [ linux-4.17.19 ] ~ [ linux-4.16.18 ] ~ [ linux-4.15.18 ] ~ [ linux-4.14.336 ] ~ [ linux-4.13.16 ] ~ [ linux-4.12.14 ] ~ [ linux-4.11.12 ] ~ [ linux-4.10.17 ] ~ [ linux-4.9.337 ] ~ [ linux-4.4.302 ] ~ [ linux-3.10.108 ] ~ [ linux-2.6.32.71 ] ~ [ linux-2.6.0 ] ~ [ linux-2.4.37.11 ] ~ [ unix-v6-master ] ~ [ ccs-tools-1.8.12 ] ~ [ policy-sample ] ~
Architecture: ~ [ i386 ] ~ [ alpha ] ~ [ m68k ] ~ [ mips ] ~ [ ppc ] ~ [ sparc ] ~ [ sparc64 ] ~

Diff markup

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 12 << 13 LDFLAGS_vmlinux :=--no-undefined -X --pic-vene << 14 << 15 ifeq ($(CONFIG_RELOCATABLE), y) << 16 # Pass --no-apply-dynamic-relocs to restore pr << 17 # for relative relocs, since this leads to bet << 18 # with the relocation offsets always being zer << 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 << 91 # Tell the assembler to support instructions f << 92 # architecture. << 93 # 9 # 94 # For non-integrated assemblers we'll pass thi << 95 # integrated assemblers we'll define ARM64_ASM << 96 # inline usage. << 97 # << 98 # We cannot pass the same arch flag to the com << 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 10 177 all: $(notdir $(KBUILD_IMAGE)) !! 11 NM := $(NM) -B 178 12 179 image.fit: dtbs !! 13 LDFLAGS_vmlinux := -static -N #-relax >> 14 CHECKFLAGS += -D__alpha__ >> 15 cflags-y := -pipe -mno-fp-regs -ffixed-8 >> 16 cflags-y += $(call cc-option, -fno-jump-tables) >> 17 >> 18 cpuflags-$(CONFIG_ALPHA_EV4) := -mcpu=ev4 >> 19 cpuflags-$(CONFIG_ALPHA_EV5) := -mcpu=ev5 >> 20 cpuflags-$(CONFIG_ALPHA_EV56) := -mcpu=ev56 >> 21 cpuflags-$(CONFIG_ALPHA_POLARIS) := -mcpu=pca56 >> 22 cpuflags-$(CONFIG_ALPHA_SX164) := -mcpu=pca56 >> 23 cpuflags-$(CONFIG_ALPHA_EV6) := -mcpu=ev6 >> 24 cpuflags-$(CONFIG_ALPHA_EV67) := -mcpu=ev67 >> 25 # If GENERIC, make sure to turn off any instruction set extensions that >> 26 # the host compiler might have on by default. Given that EV4 and EV5 >> 27 # have the same instruction set, prefer EV5 because an EV5 schedule is >> 28 # more likely to keep an EV4 processor busy than vice-versa. >> 29 cpuflags-$(CONFIG_ALPHA_GENERIC) := -mcpu=ev5 >> 30 >> 31 cflags-y += $(cpuflags-y) >> 32 >> 33 >> 34 # For TSUNAMI, we must have the assembler not emulate our instructions. >> 35 # The same is true for IRONGATE, POLARIS, PYXIS. >> 36 # BWX is most important, but we don't really want any emulation ever. >> 37 KBUILD_CFLAGS += $(cflags-y) -Wa,-mev6 >> 38 >> 39 head-y := arch/alpha/kernel/head.o >> 40 >> 41 core-y += arch/alpha/kernel/ arch/alpha/mm/ >> 42 core-$(CONFIG_MATHEMU) += arch/alpha/math-emu/ >> 43 drivers-$(CONFIG_OPROFILE) += arch/alpha/oprofile/ >> 44 libs-y += arch/alpha/lib/ >> 45 >> 46 # export what is needed by arch/alpha/boot/Makefile >> 47 LIBS_Y := $(patsubst %/, %/lib.a, $(libs-y)) >> 48 export LIBS_Y >> 49 >> 50 boot := arch/alpha/boot 180 51 181 vmlinuz.efi image.fit: Image !! 52 #Default target when executing make with no arguments 182 $(BOOT_TARGETS): vmlinux !! 53 all boot: $(boot)/vmlinux.gz 183 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ !! 54 >> 55 $(boot)/vmlinux.gz: vmlinux >> 56 $(Q)$(MAKE) $(build)=$(boot) $@ 184 57 185 Image.%: Image !! 58 bootimage bootpfile bootpzfile: vmlinux 186 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ 59 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$@ 187 60 188 ifeq ($(CONFIG_COMPRESSED_INSTALL),y) !! 61 archclean: 189 DEFAULT_KBUILD_IMAGE = $(KBUILD_IMAGE) !! 62 $(Q)$(MAKE) $(clean)=$(boot) 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 63 237 define archhelp 64 define archhelp 238 echo '* Image.gz - Compressed kernel i !! 65 echo '* boot - Compressed kernel image (arch/alpha/boot/vmlinux.gz)' 239 echo ' Image - Uncompressed kernel !! 66 echo ' bootimage - SRM bootable image (arch/alpha/boot/bootimage)' 240 echo ' image.fit - Flat Image Tree (ar !! 67 echo ' bootpfile - BOOTP bootable image (arch/alpha/boot/bootpfile)' 241 echo ' install - Install kernel (com !! 68 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 69 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.

TOMOYO Linux Cross Reference
Linux/arch/arm64/Makefile

Diff markup

Differences between /arch/arm64/Makefile (Version linux-6.12-rc7) and /arch/alpha/Makefile (Version linux-4.19.323)

TOMOYO Linux Cross Reference Linux/arch/arm64/Makefile

Diff markup

Differences between /arch/arm64/Makefile (Version linux-6.12-rc7) and /arch/alpha/Makefile (Version linux-4.19.323)

TOMOYO Linux Cross Reference
Linux/arch/arm64/Makefile