1 # 1 #
2 # arch/arm64/Makefile <<
3 # <<
4 # This file is included by the global makefile <<
5 # architecture-specific flags and dependencies <<
6 # <<
7 # This file is subject to the terms and condit 2 # This file is subject to the terms and conditions of the GNU General Public
8 # License. See the file "COPYING" in the main 3 # License. See the file "COPYING" in the main directory of this archive
9 # for more details. 4 # for more details.
10 # 5 #
11 # Copyright (C) 1995-2001 by Russell King !! 6 # Copyright (C) 1994, 95, 96, 2003 by Ralf Baechle
>> 7 # DECStation modifications by Paul M. Antoine, 1996
>> 8 # Copyright (C) 2002, 2003, 2004 Maciej W. Rozycki
>> 9 #
>> 10 # This file is included by the global makefile so that you can add your own
>> 11 # architecture-specific flags and dependencies. Remember to do have actions
>> 12 # for "archclean" cleaning up for this architecture.
>> 13 #
12 14
13 LDFLAGS_vmlinux :=--no-undefined -X --pic-vene !! 15 KBUILD_DEFCONFIG := ip22_defconfig
14 16
15 ifeq ($(CONFIG_RELOCATABLE), y) !! 17 #
16 # Pass --no-apply-dynamic-relocs to restore pr !! 18 # Select the object file format to substitute into the linker script.
17 # for relative relocs, since this leads to bet !! 19 #
18 # with the relocation offsets always being zer !! 20 ifdef CONFIG_CPU_LITTLE_ENDIAN
19 LDFLAGS_vmlinux += -shared -Bsymbolic !! 21 32bit-tool-archpref = mipsel
20 $(call ld-option, --no !! 22 64bit-tool-archpref = mips64el
>> 23 32bit-bfd = elf32-tradlittlemips
>> 24 64bit-bfd = elf64-tradlittlemips
>> 25 32bit-emul = elf32ltsmip
>> 26 64bit-emul = elf64ltsmip
>> 27 else
>> 28 32bit-tool-archpref = mips
>> 29 64bit-tool-archpref = mips64
>> 30 32bit-bfd = elf32-tradbigmips
>> 31 64bit-bfd = elf64-tradbigmips
>> 32 32bit-emul = elf32btsmip
>> 33 64bit-emul = elf64btsmip
>> 34 endif
>> 35
>> 36 ifdef CONFIG_32BIT
>> 37 tool-archpref = $(32bit-tool-archpref)
>> 38 UTS_MACHINE := mips
>> 39 endif
>> 40 ifdef CONFIG_64BIT
>> 41 tool-archpref = $(64bit-tool-archpref)
>> 42 UTS_MACHINE := mips64
>> 43 endif
>> 44
>> 45 ifneq ($(SUBARCH),$(ARCH))
>> 46 ifeq ($(CROSS_COMPILE),)
>> 47 CROSS_COMPILE := $(call cc-cross-prefix, $(tool-archpref)-linux- $(tool-archpref)-linux-gnu- $(tool-archpref)-unknown-linux-gnu-)
>> 48 endif
21 endif 49 endif
22 50
23 ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) !! 51 cflags-y := -ffunction-sections
24 ifeq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_8434 !! 52 cflags-y += $(call cc-option, -mno-check-zero-division)
25 LDFLAGS_vmlinux += --fix-cortex-a53-843419 !! 53
26 endif !! 54 ifdef CONFIG_32BIT
>> 55 ld-emul = $(32bit-emul)
>> 56 vmlinux-32 = vmlinux
>> 57 vmlinux-64 = vmlinux.64
>> 58
>> 59 cflags-y += -mabi=32
27 endif 60 endif
28 61
29 cc_has_k_constraint := $(call try-run,echo !! 62 ifdef CONFIG_64BIT
30 'int main(void) { !! 63 ld-emul = $(64bit-emul)
31 asm volatile("and w0, w0, %w0" !! 64 vmlinux-32 = vmlinux.32
32 return 0; !! 65 vmlinux-64 = vmlinux
33 }' | $(CC) -S -x c -o "$$TMP" -,,-DCON !! 66
34 !! 67 cflags-y += -mabi=64
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 68 endif
90 69
91 # Tell the assembler to support instructions f !! 70 all-$(CONFIG_BOOT_ELF32) := $(vmlinux-32)
92 # architecture. !! 71 all-$(CONFIG_BOOT_ELF64) := $(vmlinux-64)
>> 72
93 # 73 #
94 # For non-integrated assemblers we'll pass thi !! 74 # GCC uses -G 0 -mabicalls -fpic as default. We don't want PIC in the kernel
95 # integrated assemblers we'll define ARM64_ASM !! 75 # code since it only slows down the whole thing. At some point we might make
96 # inline usage. !! 76 # use of global pointer optimizations but their use of $28 conflicts with
97 # !! 77 # the current pointer optimization.
98 # We cannot pass the same arch flag to the com !! 78 #
99 # freely generate instructions which are not s !! 79 # The DECStation requires an ECOFF kernel for remote booting, other MIPS
100 # versions, which would prevent a single kerne !! 80 # machines may also. Since BFD is incredibly buggy with respect to
101 # hardware. !! 81 # crossformat linking we rely on the elf2ecoff tool for format conversion.
102 ifeq ($(CONFIG_AS_HAS_ARMV8_5), y) !! 82 #
103 asm-arch := armv8.5-a !! 83 cflags-y += -G 0 -mno-abicalls -fno-pic -pipe
104 else ifeq ($(CONFIG_AS_HAS_ARMV8_4), y) !! 84 cflags-y += -msoft-float
105 asm-arch := armv8.4-a !! 85 LDFLAGS_vmlinux += -G 0 -static -n -nostdlib
106 else ifeq ($(CONFIG_AS_HAS_ARMV8_3), y) !! 86 MODFLAGS += -mlong-calls
107 asm-arch := armv8.3-a !! 87
108 else ifeq ($(CONFIG_AS_HAS_ARMV8_2), y) !! 88 cflags-y += -ffreestanding
109 asm-arch := armv8.2-a !! 89
110 endif !! 90 #
111 !! 91 # We explicitly add the endianness specifier if needed, this allows
112 ifdef asm-arch !! 92 # to compile kernels with a toolchain for the other endianness. We
113 KBUILD_CFLAGS += -Wa,-march=$(asm-arch) \ !! 93 # carefully avoid to add it redundantly because gcc 3.3/3.4 complains
114 -DARM64_ASM_ARCH='"$(asm-ar !! 94 # when fed the toolchain default!
115 endif !! 95 #
116 !! 96 # Certain gcc versions upto gcc 4.1.1 (probably 4.2-subversion as of
117 ifeq ($(CONFIG_SHADOW_CALL_STACK), y) !! 97 # 2006-10-10 don't properly change the predefined symbols if -EB / -EL
118 KBUILD_CFLAGS += -ffixed-x18 !! 98 # are used, so we kludge that here. A bug has been filed at
119 KBUILD_RUSTFLAGS += -Zfixed-x18 !! 99 # http://gcc.gnu.org/bugzilla/show_bug.cgi?id=29413.
120 endif !! 100 #
121 !! 101 undef-all += -UMIPSEB -U_MIPSEB -U__MIPSEB -U__MIPSEB__
122 ifeq ($(CONFIG_CPU_BIG_ENDIAN), y) !! 102 undef-all += -UMIPSEL -U_MIPSEL -U__MIPSEL -U__MIPSEL__
123 KBUILD_CPPFLAGS += -mbig-endian !! 103 predef-be += -DMIPSEB -D_MIPSEB -D__MIPSEB -D__MIPSEB__
124 CHECKFLAGS += -D__AARCH64EB__ !! 104 predef-le += -DMIPSEL -D_MIPSEL -D__MIPSEL -D__MIPSEL__
125 # Prefer the baremetal ELF build target, but n !! 105 cflags-$(CONFIG_CPU_BIG_ENDIAN) += $(shell $(CC) -dumpmachine |grep -q 'mips.*el-.*' && echo -EB $(undef-all) $(predef-be))
126 # it so fall back to the standard linux versio !! 106 cflags-$(CONFIG_CPU_LITTLE_ENDIAN) += $(shell $(CC) -dumpmachine |grep -q 'mips.*el-.*' || echo -EL $(undef-all) $(predef-le))
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 107
137 ifeq ($(CONFIG_LD_IS_LLD), y) !! 108 cflags-$(CONFIG_CPU_HAS_SMARTMIPS) += $(call cc-option,-msmartmips)
138 KBUILD_LDFLAGS += -z norelro !! 109
>> 110 cflags-$(CONFIG_SB1XXX_CORELIS) += $(call cc-option,-mno-sched-prolog) \
>> 111 -fno-omit-frame-pointer
>> 112
>> 113 #
>> 114 # CPU-dependent compiler/assembler options for optimization.
>> 115 #
>> 116 cflags-$(CONFIG_CPU_R3000) += -march=r3000
>> 117 cflags-$(CONFIG_CPU_TX39XX) += -march=r3900
>> 118 cflags-$(CONFIG_CPU_R6000) += -march=r6000 -Wa,--trap
>> 119 cflags-$(CONFIG_CPU_R4300) += -march=r4300 -Wa,--trap
>> 120 cflags-$(CONFIG_CPU_VR41XX) += -march=r4100 -Wa,--trap
>> 121 cflags-$(CONFIG_CPU_R4X00) += -march=r4600 -Wa,--trap
>> 122 cflags-$(CONFIG_CPU_TX49XX) += -march=r4600 -Wa,--trap
>> 123 # only gcc >= 4.4 have the loongson-specific support
>> 124 cflags-$(CONFIG_CPU_LOONGSON2) += -Wa,--trap
>> 125 cflags-$(CONFIG_CPU_LOONGSON2E) += \
>> 126 $(call cc-option,-march=loongson2e,-march=r4600)
>> 127
>> 128 cflags-$(CONFIG_CPU_MIPS32_R1) += $(call cc-option,-march=mips32,-mips32 -U_MIPS_ISA -D_MIPS_ISA=_MIPS_ISA_MIPS32) \
>> 129 -Wa,-mips32 -Wa,--trap
>> 130 cflags-$(CONFIG_CPU_MIPS32_R2) += $(call cc-option,-march=mips32r2,-mips32r2 -U_MIPS_ISA -D_MIPS_ISA=_MIPS_ISA_MIPS32) \
>> 131 -Wa,-mips32r2 -Wa,--trap
>> 132 cflags-$(CONFIG_CPU_MIPS64_R1) += $(call cc-option,-march=mips64,-mips64 -U_MIPS_ISA -D_MIPS_ISA=_MIPS_ISA_MIPS64) \
>> 133 -Wa,-mips64 -Wa,--trap
>> 134 cflags-$(CONFIG_CPU_MIPS64_R2) += $(call cc-option,-march=mips64r2,-mips64r2 -U_MIPS_ISA -D_MIPS_ISA=_MIPS_ISA_MIPS64) \
>> 135 -Wa,-mips64r2 -Wa,--trap
>> 136 cflags-$(CONFIG_CPU_R5000) += -march=r5000 -Wa,--trap
>> 137 cflags-$(CONFIG_CPU_R5432) += $(call cc-option,-march=r5400,-march=r5000) \
>> 138 -Wa,--trap
>> 139 cflags-$(CONFIG_CPU_R5500) += $(call cc-option,-march=r5500,-march=r5000) \
>> 140 -Wa,--trap
>> 141 cflags-$(CONFIG_CPU_NEVADA) += $(call cc-option,-march=rm5200,-march=r5000) \
>> 142 -Wa,--trap
>> 143 cflags-$(CONFIG_CPU_RM7000) += $(call cc-option,-march=rm7000,-march=r5000) \
>> 144 -Wa,--trap
>> 145 cflags-$(CONFIG_CPU_RM9000) += $(call cc-option,-march=rm9000,-march=r5000) \
>> 146 -Wa,--trap
>> 147 cflags-$(CONFIG_CPU_SB1) += $(call cc-option,-march=sb1,-march=r5000) \
>> 148 -Wa,--trap
>> 149 cflags-$(CONFIG_CPU_R8000) += -march=r8000 -Wa,--trap
>> 150 cflags-$(CONFIG_CPU_R10000) += $(call cc-option,-march=r10000,-march=r8000) \
>> 151 -Wa,--trap
>> 152 cflags-$(CONFIG_CPU_CAVIUM_OCTEON) += $(call cc-option,-march=octeon) -Wa,--trap
>> 153 ifeq (,$(findstring march=octeon, $(cflags-$(CONFIG_CPU_CAVIUM_OCTEON))))
>> 154 cflags-$(CONFIG_CPU_CAVIUM_OCTEON) += -Wa,-march=octeon
>> 155 endif
>> 156
>> 157 cflags-$(CONFIG_CPU_R4000_WORKAROUNDS) += $(call cc-option,-mfix-r4000,)
>> 158 cflags-$(CONFIG_CPU_R4400_WORKAROUNDS) += $(call cc-option,-mfix-r4400,)
>> 159 cflags-$(CONFIG_CPU_DADDI_WORKAROUNDS) += $(call cc-option,-mno-daddi,)
>> 160
>> 161 ifdef CONFIG_CPU_SB1
>> 162 ifdef CONFIG_SB1_PASS_1_WORKAROUNDS
>> 163 MODFLAGS += -msb1-pass1-workarounds
139 endif 164 endif
>> 165 endif
>> 166
>> 167 #
>> 168 # Firmware support
>> 169 #
>> 170 libs-$(CONFIG_ARC) += arch/mips/fw/arc/
>> 171 libs-$(CONFIG_CFE) += arch/mips/fw/cfe/
>> 172 libs-$(CONFIG_SNIPROM) += arch/mips/fw/sni/
>> 173 libs-y += arch/mips/fw/lib/
>> 174
>> 175 #
>> 176 # Board-dependent options and extra files
>> 177 #
>> 178
>> 179 #
>> 180 # Texas Instruments AR7
>> 181 #
>> 182 core-$(CONFIG_AR7) += arch/mips/ar7/
>> 183 cflags-$(CONFIG_AR7) += -I$(srctree)/arch/mips/include/asm/mach-ar7
>> 184 load-$(CONFIG_AR7) += 0xffffffff94100000
>> 185
>> 186 #
>> 187 # Acer PICA 61, Mips Magnum 4000 and Olivetti M700.
>> 188 #
>> 189 core-$(CONFIG_MACH_JAZZ) += arch/mips/jazz/
>> 190 cflags-$(CONFIG_MACH_JAZZ) += -I$(srctree)/arch/mips/include/asm/mach-jazz
>> 191 load-$(CONFIG_MACH_JAZZ) += 0xffffffff80080000
>> 192
>> 193 #
>> 194 # Common Alchemy Au1x00 stuff
>> 195 #
>> 196 core-$(CONFIG_SOC_AU1X00) += arch/mips/alchemy/common/
>> 197
>> 198 #
>> 199 # AMD Alchemy Pb1000 eval board
>> 200 #
>> 201 core-$(CONFIG_MIPS_PB1000) += arch/mips/alchemy/devboards/
>> 202 cflags-$(CONFIG_MIPS_PB1000) += -I$(srctree)/arch/mips/include/asm/mach-pb1x00
>> 203 load-$(CONFIG_MIPS_PB1000) += 0xffffffff80100000
>> 204
>> 205 #
>> 206 # AMD Alchemy Pb1100 eval board
>> 207 #
>> 208 core-$(CONFIG_MIPS_PB1100) += arch/mips/alchemy/devboards/
>> 209 cflags-$(CONFIG_MIPS_PB1100) += -I$(srctree)/arch/mips/include/asm/mach-pb1x00
>> 210 load-$(CONFIG_MIPS_PB1100) += 0xffffffff80100000
>> 211
>> 212 #
>> 213 # AMD Alchemy Pb1500 eval board
>> 214 #
>> 215 core-$(CONFIG_MIPS_PB1500) += arch/mips/alchemy/devboards/
>> 216 cflags-$(CONFIG_MIPS_PB1500) += -I$(srctree)/arch/mips/include/asm/mach-pb1x00
>> 217 load-$(CONFIG_MIPS_PB1500) += 0xffffffff80100000
>> 218
>> 219 #
>> 220 # AMD Alchemy Pb1550 eval board
>> 221 #
>> 222 core-$(CONFIG_MIPS_PB1550) += arch/mips/alchemy/devboards/
>> 223 cflags-$(CONFIG_MIPS_PB1550) += -I$(srctree)/arch/mips/include/asm/mach-pb1x00
>> 224 load-$(CONFIG_MIPS_PB1550) += 0xffffffff80100000
>> 225
>> 226 #
>> 227 # AMD Alchemy Pb1200 eval board
>> 228 #
>> 229 core-$(CONFIG_MIPS_PB1200) += arch/mips/alchemy/devboards/
>> 230 cflags-$(CONFIG_MIPS_PB1200) += -I$(srctree)/arch/mips/include/asm/mach-pb1x00
>> 231 load-$(CONFIG_MIPS_PB1200) += 0xffffffff80100000
>> 232
>> 233 #
>> 234 # AMD Alchemy Db1000 eval board
>> 235 #
>> 236 core-$(CONFIG_MIPS_DB1000) += arch/mips/alchemy/devboards/
>> 237 cflags-$(CONFIG_MIPS_DB1000) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 238 load-$(CONFIG_MIPS_DB1000) += 0xffffffff80100000
>> 239
>> 240 #
>> 241 # AMD Alchemy Db1100 eval board
>> 242 #
>> 243 core-$(CONFIG_MIPS_DB1100) += arch/mips/alchemy/devboards/
>> 244 cflags-$(CONFIG_MIPS_DB1100) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 245 load-$(CONFIG_MIPS_DB1100) += 0xffffffff80100000
>> 246
>> 247 #
>> 248 # AMD Alchemy Db1500 eval board
>> 249 #
>> 250 core-$(CONFIG_MIPS_DB1500) += arch/mips/alchemy/devboards/
>> 251 cflags-$(CONFIG_MIPS_DB1500) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 252 load-$(CONFIG_MIPS_DB1500) += 0xffffffff80100000
>> 253
>> 254 #
>> 255 # AMD Alchemy Db1550 eval board
>> 256 #
>> 257 core-$(CONFIG_MIPS_DB1550) += arch/mips/alchemy/devboards/
>> 258 cflags-$(CONFIG_MIPS_DB1550) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 259 load-$(CONFIG_MIPS_DB1550) += 0xffffffff80100000
>> 260
>> 261 #
>> 262 # AMD Alchemy Db1200 eval board
>> 263 #
>> 264 core-$(CONFIG_MIPS_DB1200) += arch/mips/alchemy/devboards/
>> 265 cflags-$(CONFIG_MIPS_DB1200) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 266 load-$(CONFIG_MIPS_DB1200) += 0xffffffff80100000
>> 267
>> 268 #
>> 269 # AMD Alchemy Bosporus eval board
>> 270 #
>> 271 core-$(CONFIG_MIPS_BOSPORUS) += arch/mips/alchemy/devboards/
>> 272 cflags-$(CONFIG_MIPS_BOSPORUS) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 273 load-$(CONFIG_MIPS_BOSPORUS) += 0xffffffff80100000
>> 274
>> 275 #
>> 276 # AMD Alchemy Mirage eval board
>> 277 #
>> 278 core-$(CONFIG_MIPS_MIRAGE) += arch/mips/alchemy/devboards/
>> 279 cflags-$(CONFIG_MIPS_MIRAGE) += -I$(srctree)/arch/mips/include/asm/mach-db1x00
>> 280 load-$(CONFIG_MIPS_MIRAGE) += 0xffffffff80100000
140 281
141 CHECKFLAGS += -D__aarch64__ !! 282 #
>> 283 # 4G-Systems eval board
>> 284 #
>> 285 libs-$(CONFIG_MIPS_MTX1) += arch/mips/alchemy/mtx-1/
>> 286 load-$(CONFIG_MIPS_MTX1) += 0xffffffff80100000
>> 287
>> 288 #
>> 289 # MyCable eval board
>> 290 #
>> 291 libs-$(CONFIG_MIPS_XXS1500) += arch/mips/alchemy/xxs1500/
>> 292 load-$(CONFIG_MIPS_XXS1500) += 0xffffffff80100000
>> 293
>> 294 # must be last for Alchemy systems for GPIO to work properly
>> 295 cflags-$(CONFIG_SOC_AU1X00) += -I$(srctree)/arch/mips/include/asm/mach-au1x00
>> 296
>> 297
>> 298 #
>> 299 # Cobalt Server
>> 300 #
>> 301 core-$(CONFIG_MIPS_COBALT) += arch/mips/cobalt/
>> 302 cflags-$(CONFIG_MIPS_COBALT) += -I$(srctree)/arch/mips/include/asm/mach-cobalt
>> 303 load-$(CONFIG_MIPS_COBALT) += 0xffffffff80080000
>> 304
>> 305 #
>> 306 # DECstation family
>> 307 #
>> 308 core-$(CONFIG_MACH_DECSTATION) += arch/mips/dec/
>> 309 cflags-$(CONFIG_MACH_DECSTATION)+= -I$(srctree)/arch/mips/include/asm/mach-dec
>> 310 libs-$(CONFIG_MACH_DECSTATION) += arch/mips/dec/prom/
>> 311 load-$(CONFIG_MACH_DECSTATION) += 0xffffffff80040000
>> 312
>> 313 #
>> 314 # Wind River PPMC Board (4KC + GT64120)
>> 315 #
>> 316 core-$(CONFIG_WR_PPMC) += arch/mips/gt64120/wrppmc/
>> 317 cflags-$(CONFIG_WR_PPMC) += -I$(srctree)/arch/mips/include/asm/mach-wrppmc
>> 318 load-$(CONFIG_WR_PPMC) += 0xffffffff80100000
>> 319
>> 320 #
>> 321 # Loongson family
>> 322 #
>> 323 core-$(CONFIG_MACH_LOONGSON) +=arch/mips/loongson/
>> 324 cflags-$(CONFIG_MACH_LOONGSON) += -I$(srctree)/arch/mips/include/asm/mach-loongson \
>> 325 -mno-branch-likely
>> 326 load-$(CONFIG_LEMOTE_FULOONG2E) +=0xffffffff80100000
>> 327
>> 328 #
>> 329 # MIPS Malta board
>> 330 #
>> 331 core-$(CONFIG_MIPS_MALTA) += arch/mips/mti-malta/
>> 332 cflags-$(CONFIG_MIPS_MALTA) += -I$(srctree)/arch/mips/include/asm/mach-malta
>> 333 load-$(CONFIG_MIPS_MALTA) += 0xffffffff80100000
>> 334 all-$(CONFIG_MIPS_MALTA) := vmlinux.bin
>> 335
>> 336 #
>> 337 # MIPS SIM
>> 338 #
>> 339 core-$(CONFIG_MIPS_SIM) += arch/mips/mipssim/
>> 340 cflags-$(CONFIG_MIPS_SIM) += -I$(srctree)/arch/mips/include/asm/mach-mipssim
>> 341 load-$(CONFIG_MIPS_SIM) += 0x80100000
>> 342
>> 343 #
>> 344 # PMC-Sierra MSP SOCs
>> 345 #
>> 346 core-$(CONFIG_PMC_MSP) += arch/mips/pmc-sierra/msp71xx/
>> 347 cflags-$(CONFIG_PMC_MSP) += -I$(srctree)/arch/mips/include/asm/pmc-sierra/msp71xx \
>> 348 -mno-branch-likely
>> 349 load-$(CONFIG_PMC_MSP) += 0xffffffff80100000
142 350
143 ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_CALL_OPS),y !! 351 #
144 KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNC !! 352 # PMC-Sierra Yosemite
145 CC_FLAGS_FTRACE := -fpatchable-function-entr !! 353 #
146 else ifeq ($(CONFIG_DYNAMIC_FTRACE_WITH_ARGS), !! 354 core-$(CONFIG_PMC_YOSEMITE) += arch/mips/pmc-sierra/yosemite/
147 KBUILD_CPPFLAGS += -DCC_USING_PATCHABLE_FUNC !! 355 cflags-$(CONFIG_PMC_YOSEMITE) += -I$(srctree)/arch/mips/include/asm/mach-yosemite
148 CC_FLAGS_FTRACE := -fpatchable-function-entr !! 356 load-$(CONFIG_PMC_YOSEMITE) += 0xffffffff80100000
>> 357
>> 358 #
>> 359 # Basler eXcite
>> 360 #
>> 361 core-$(CONFIG_BASLER_EXCITE) += arch/mips/basler/excite/
>> 362 cflags-$(CONFIG_BASLER_EXCITE) += -I$(srctree)/arch/mips/include/asm/mach-excite
>> 363 load-$(CONFIG_BASLER_EXCITE) += 0x80100000
>> 364
>> 365 #
>> 366 # LASAT platforms
>> 367 #
>> 368 core-$(CONFIG_LASAT) += arch/mips/lasat/
>> 369 cflags-$(CONFIG_LASAT) += -I$(srctree)/arch/mips/include/asm/mach-lasat
>> 370 load-$(CONFIG_LASAT) += 0xffffffff80000000
>> 371
>> 372 #
>> 373 # Common VR41xx
>> 374 #
>> 375 core-$(CONFIG_MACH_VR41XX) += arch/mips/vr41xx/common/
>> 376 cflags-$(CONFIG_MACH_VR41XX) += -I$(srctree)/arch/mips/include/asm/mach-vr41xx
>> 377
>> 378 #
>> 379 # ZAO Networks Capcella (VR4131)
>> 380 #
>> 381 load-$(CONFIG_ZAO_CAPCELLA) += 0xffffffff80000000
>> 382
>> 383 #
>> 384 # Victor MP-C303/304 (VR4122)
>> 385 #
>> 386 load-$(CONFIG_VICTOR_MPC30X) += 0xffffffff80001000
>> 387
>> 388 #
>> 389 # IBM WorkPad z50 (VR4121)
>> 390 #
>> 391 core-$(CONFIG_IBM_WORKPAD) += arch/mips/vr41xx/ibm-workpad/
>> 392 load-$(CONFIG_IBM_WORKPAD) += 0xffffffff80004000
>> 393
>> 394 #
>> 395 # CASIO CASSIPEIA E-55/65 (VR4111)
>> 396 #
>> 397 core-$(CONFIG_CASIO_E55) += arch/mips/vr41xx/casio-e55/
>> 398 load-$(CONFIG_CASIO_E55) += 0xffffffff80004000
>> 399
>> 400 #
>> 401 # TANBAC VR4131 multichip module(TB0225) and TANBAC VR4131DIMM(TB0229) (VR4131)
>> 402 #
>> 403 load-$(CONFIG_TANBAC_TB022X) += 0xffffffff80000000
>> 404
>> 405 # NXP STB225
>> 406 core-$(CONFIG_SOC_PNX833X) += arch/mips/nxp/pnx833x/common/
>> 407 cflags-$(CONFIG_SOC_PNX833X) += -Iarch/mips/include/asm/mach-pnx833x
>> 408 libs-$(CONFIG_NXP_STB220) += arch/mips/nxp/pnx833x/stb22x/
>> 409 load-$(CONFIG_NXP_STB220) += 0xffffffff80001000
>> 410 libs-$(CONFIG_NXP_STB225) += arch/mips/nxp/pnx833x/stb22x/
>> 411 load-$(CONFIG_NXP_STB225) += 0xffffffff80001000
>> 412
>> 413 #
>> 414 # Common NXP PNX8550
>> 415 #
>> 416 core-$(CONFIG_SOC_PNX8550) += arch/mips/nxp/pnx8550/common/
>> 417 cflags-$(CONFIG_SOC_PNX8550) += -I$(srctree)/arch/mips/include/asm/mach-pnx8550
>> 418
>> 419 #
>> 420 # NXP PNX8550 JBS board
>> 421 #
>> 422 libs-$(CONFIG_PNX8550_JBS) += arch/mips/nxp/pnx8550/jbs/
>> 423 #cflags-$(CONFIG_PNX8550_JBS) += -I$(srctree)/arch/mips/include/asm/mach-pnx8550
>> 424 load-$(CONFIG_PNX8550_JBS) += 0xffffffff80060000
>> 425
>> 426 # NXP PNX8550 STB810 board
>> 427 #
>> 428 libs-$(CONFIG_PNX8550_STB810) += arch/mips/nxp/pnx8550/stb810/
>> 429 load-$(CONFIG_PNX8550_STB810) += 0xffffffff80060000
>> 430
>> 431 #
>> 432 # Common NEC EMMAXXX
>> 433 #
>> 434 core-$(CONFIG_SOC_EMMA2RH) += arch/mips/emma/common/
>> 435 cflags-$(CONFIG_SOC_EMMA2RH) += -I$(srctree)/arch/mips/include/asm/mach-emma2rh
>> 436
>> 437 #
>> 438 # NEC EMMA2RH Mark-eins
>> 439 #
>> 440 core-$(CONFIG_NEC_MARKEINS) += arch/mips/emma/markeins/
>> 441 load-$(CONFIG_NEC_MARKEINS) += 0xffffffff88100000
>> 442
>> 443 #
>> 444 # SGI IP22 (Indy/Indigo2)
>> 445 #
>> 446 # Set the load address to >= 0xffffffff88069000 if you want to leave space for
>> 447 # symmon, 0xffffffff80002000 for production kernels. Note that the value must
>> 448 # be aligned to a multiple of the kernel stack size or the handling of the
>> 449 # current variable will break so for 64-bit kernels we have to raise the start
>> 450 # address by 8kb.
>> 451 #
>> 452 core-$(CONFIG_SGI_IP22) += arch/mips/sgi-ip22/
>> 453 cflags-$(CONFIG_SGI_IP22) += -I$(srctree)/arch/mips/include/asm/mach-ip22
>> 454 ifdef CONFIG_32BIT
>> 455 load-$(CONFIG_SGI_IP22) += 0xffffffff88002000
>> 456 endif
>> 457 ifdef CONFIG_64BIT
>> 458 load-$(CONFIG_SGI_IP22) += 0xffffffff88004000
149 endif 459 endif
150 460
151 ifeq ($(CONFIG_KASAN_SW_TAGS), y) !! 461 #
152 KASAN_SHADOW_SCALE_SHIFT := 4 !! 462 # SGI-IP27 (Origin200/2000)
153 else ifeq ($(CONFIG_KASAN_GENERIC), y) !! 463 #
154 KASAN_SHADOW_SCALE_SHIFT := 3 !! 464 # Set the load address to >= 0xc000000000300000 if you want to leave space for
>> 465 # symmon, 0xc00000000001c000 for production kernels. Note that the value must
>> 466 # be 16kb aligned or the handling of the current variable will break.
>> 467 #
>> 468 ifdef CONFIG_SGI_IP27
>> 469 core-$(CONFIG_SGI_IP27) += arch/mips/sgi-ip27/
>> 470 cflags-$(CONFIG_SGI_IP27) += -I$(srctree)/arch/mips/include/asm/mach-ip27
>> 471 ifdef CONFIG_MAPPED_KERNEL
>> 472 load-$(CONFIG_SGI_IP27) += 0xc00000004001c000
>> 473 OBJCOPYFLAGS := --change-addresses=0x3fffffff80000000
>> 474 dataoffset-$(CONFIG_SGI_IP27) += 0x01000000
>> 475 else
>> 476 load-$(CONFIG_SGI_IP27) += 0xa80000000001c000
>> 477 OBJCOPYFLAGS := --change-addresses=0x57ffffff80000000
>> 478 endif
155 endif 479 endif
156 480
157 KBUILD_CFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$( !! 481 #
158 KBUILD_CPPFLAGS += -DKASAN_SHADOW_SCALE_SHIFT= !! 482 # SGI IP28 (Indigo2 R10k)
159 KBUILD_AFLAGS += -DKASAN_SHADOW_SCALE_SHIFT=$( !! 483 #
>> 484 # Set the load address to >= 0xa800000020080000 if you want to leave space for
>> 485 # symmon, 0xa800000020004000 for production kernels ? Note that the value must
>> 486 # be 16kb aligned or the handling of the current variable will break.
>> 487 # Simplified: what IP22 does at 128MB+ in ksegN, IP28 does at 512MB+ in xkphys
>> 488 #
>> 489 ifdef CONFIG_SGI_IP28
>> 490 ifeq ($(call cc-option-yn,-mr10k-cache-barrier=store), n)
>> 491 $(error gcc doesn't support needed option -mr10k-cache-barrier=store)
>> 492 endif
>> 493 endif
>> 494 core-$(CONFIG_SGI_IP28) += arch/mips/sgi-ip22/
>> 495 cflags-$(CONFIG_SGI_IP28) += -mr10k-cache-barrier=store -I$(srctree)/arch/mips/include/asm/mach-ip28
>> 496 load-$(CONFIG_SGI_IP28) += 0xa800000020004000
160 497
161 libs-y := arch/arm64/lib/ $(libs-y) !! 498 #
162 libs-$(CONFIG_EFI_STUB) += $(objtree)/drivers/ !! 499 # SGI-IP32 (O2)
>> 500 #
>> 501 # Set the load address to >= 80069000 if you want to leave space for symmon,
>> 502 # 0xffffffff80004000 for production kernels. Note that the value must be aligned to
>> 503 # a multiple of the kernel stack size or the handling of the current variable
>> 504 # will break.
>> 505 #
>> 506 core-$(CONFIG_SGI_IP32) += arch/mips/sgi-ip32/
>> 507 cflags-$(CONFIG_SGI_IP32) += -I$(srctree)/arch/mips/include/asm/mach-ip32
>> 508 load-$(CONFIG_SGI_IP32) += 0xffffffff80004000
>> 509
>> 510 #
>> 511 # Sibyte SB1250/BCM1480 SOC
>> 512 #
>> 513 # This is a LIB so that it links at the end, and initcalls are later
>> 514 # the sequence; but it is built as an object so that modules don't get
>> 515 # removed (as happens, even if they have __initcall/module_init)
>> 516 #
>> 517 core-$(CONFIG_SIBYTE_BCM112X) += arch/mips/sibyte/sb1250/
>> 518 core-$(CONFIG_SIBYTE_BCM112X) += arch/mips/sibyte/common/
>> 519 cflags-$(CONFIG_SIBYTE_BCM112X) += -I$(srctree)/arch/mips/include/asm/mach-sibyte \
>> 520 -DSIBYTE_HDR_FEATURES=SIBYTE_HDR_FMASK_1250_112x_ALL
>> 521
>> 522 core-$(CONFIG_SIBYTE_SB1250) += arch/mips/sibyte/sb1250/
>> 523 core-$(CONFIG_SIBYTE_SB1250) += arch/mips/sibyte/common/
>> 524 cflags-$(CONFIG_SIBYTE_SB1250) += -I$(srctree)/arch/mips/include/asm/mach-sibyte \
>> 525 -DSIBYTE_HDR_FEATURES=SIBYTE_HDR_FMASK_1250_112x_ALL
>> 526
>> 527 core-$(CONFIG_SIBYTE_BCM1x55) += arch/mips/sibyte/bcm1480/
>> 528 core-$(CONFIG_SIBYTE_BCM1x55) += arch/mips/sibyte/common/
>> 529 cflags-$(CONFIG_SIBYTE_BCM1x55) += -I$(srctree)/arch/mips/include/asm/mach-sibyte \
>> 530 -DSIBYTE_HDR_FEATURES=SIBYTE_HDR_FMASK_1480_ALL
>> 531
>> 532 core-$(CONFIG_SIBYTE_BCM1x80) += arch/mips/sibyte/bcm1480/
>> 533 core-$(CONFIG_SIBYTE_BCM1x80) += arch/mips/sibyte/common/
>> 534 cflags-$(CONFIG_SIBYTE_BCM1x80) += -I$(srctree)/arch/mips/include/asm/mach-sibyte \
>> 535 -DSIBYTE_HDR_FEATURES=SIBYTE_HDR_FMASK_1480_ALL
163 536
164 # Default target when executing plain make !! 537 #
165 boot := arch/arm64/boot !! 538 # Sibyte BCM91120x (Carmel) board
>> 539 # Sibyte BCM91120C (CRhine) board
>> 540 # Sibyte BCM91125C (CRhone) board
>> 541 # Sibyte BCM91125E (Rhone) board
>> 542 # Sibyte SWARM board
>> 543 # Sibyte BCM91x80 (BigSur) board
>> 544 #
>> 545 core-$(CONFIG_SIBYTE_CARMEL) += arch/mips/sibyte/swarm/
>> 546 load-$(CONFIG_SIBYTE_CARMEL) := 0xffffffff80100000
>> 547 core-$(CONFIG_SIBYTE_CRHINE) += arch/mips/sibyte/swarm/
>> 548 load-$(CONFIG_SIBYTE_CRHINE) := 0xffffffff80100000
>> 549 core-$(CONFIG_SIBYTE_CRHONE) += arch/mips/sibyte/swarm/
>> 550 load-$(CONFIG_SIBYTE_CRHONE) := 0xffffffff80100000
>> 551 core-$(CONFIG_SIBYTE_RHONE) += arch/mips/sibyte/swarm/
>> 552 load-$(CONFIG_SIBYTE_RHONE) := 0xffffffff80100000
>> 553 core-$(CONFIG_SIBYTE_SENTOSA) += arch/mips/sibyte/swarm/
>> 554 load-$(CONFIG_SIBYTE_SENTOSA) := 0xffffffff80100000
>> 555 core-$(CONFIG_SIBYTE_SWARM) += arch/mips/sibyte/swarm/
>> 556 load-$(CONFIG_SIBYTE_SWARM) := 0xffffffff80100000
>> 557 core-$(CONFIG_SIBYTE_BIGSUR) += arch/mips/sibyte/swarm/
>> 558 load-$(CONFIG_SIBYTE_BIGSUR) := 0xffffffff80100000
166 559
167 BOOT_TARGETS := Image vmlinuz.efi image.fit !! 560 #
>> 561 # Broadcom BCM47XX boards
>> 562 #
>> 563 core-$(CONFIG_BCM47XX) += arch/mips/bcm47xx/
>> 564 cflags-$(CONFIG_BCM47XX) += -I$(srctree)/arch/mips/include/asm/mach-bcm47xx
>> 565 load-$(CONFIG_BCM47XX) := 0xffffffff80001000
168 566
169 PHONY += $(BOOT_TARGETS) !! 567 #
>> 568 # Broadcom BCM63XX boards
>> 569 #
>> 570 core-$(CONFIG_BCM63XX) += arch/mips/bcm63xx/
>> 571 cflags-$(CONFIG_BCM63XX) += -I$(srctree)/arch/mips/include/asm/mach-bcm63xx/
>> 572 load-$(CONFIG_BCM63XX) := 0xffffffff80010000
170 573
171 ifeq ($(CONFIG_EFI_ZBOOT),) !! 574 #
172 KBUILD_IMAGE := $(boot)/Image.gz !! 575 # SNI RM
>> 576 #
>> 577 core-$(CONFIG_SNI_RM) += arch/mips/sni/
>> 578 cflags-$(CONFIG_SNI_RM) += -I$(srctree)/arch/mips/include/asm/mach-rm
>> 579 ifdef CONFIG_CPU_LITTLE_ENDIAN
>> 580 load-$(CONFIG_SNI_RM) += 0xffffffff80600000
173 else 581 else
174 KBUILD_IMAGE := $(boot)/vmlinuz.efi !! 582 load-$(CONFIG_SNI_RM) += 0xffffffff80030000
175 endif 583 endif
>> 584 all-$(CONFIG_SNI_RM) := vmlinux.ecoff
176 585
177 all: $(notdir $(KBUILD_IMAGE)) !! 586 #
>> 587 # Common TXx9
>> 588 #
>> 589 core-$(CONFIG_MACH_TX39XX) += arch/mips/txx9/generic/
>> 590 cflags-$(CONFIG_MACH_TX39XX) += -I$(srctree)/arch/mips/include/asm/mach-tx39xx
>> 591 load-$(CONFIG_MACH_TX39XX) += 0xffffffff80050000
>> 592 core-$(CONFIG_MACH_TX49XX) += arch/mips/txx9/generic/
>> 593 cflags-$(CONFIG_MACH_TX49XX) += -I$(srctree)/arch/mips/include/asm/mach-tx49xx
>> 594 load-$(CONFIG_MACH_TX49XX) += 0xffffffff80100000
178 595
179 image.fit: dtbs !! 596 #
>> 597 # Toshiba JMR-TX3927 board
>> 598 #
>> 599 core-$(CONFIG_TOSHIBA_JMR3927) += arch/mips/txx9/jmr3927/
180 600
181 vmlinuz.efi image.fit: Image !! 601 #
182 $(BOOT_TARGETS): vmlinux !! 602 # Routerboard 532 board
183 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ !! 603 #
>> 604 core-$(CONFIG_MIKROTIK_RB532) += arch/mips/rb532/
>> 605 cflags-$(CONFIG_MIKROTIK_RB532) += -I$(srctree)/arch/mips/include/asm/mach-rc32434
>> 606 load-$(CONFIG_MIKROTIK_RB532) += 0xffffffff80101000
184 607
185 Image.%: Image !! 608 #
186 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ !! 609 # Toshiba RBTX49XX boards
>> 610 #
>> 611 core-$(CONFIG_TOSHIBA_RBTX4927) += arch/mips/txx9/rbtx4927/
>> 612 core-$(CONFIG_TOSHIBA_RBTX4938) += arch/mips/txx9/rbtx4938/
>> 613 core-$(CONFIG_TOSHIBA_RBTX4939) += arch/mips/txx9/rbtx4939/
187 614
188 ifeq ($(CONFIG_COMPRESSED_INSTALL),y) !! 615 #
189 DEFAULT_KBUILD_IMAGE = $(KBUILD_IMAGE) !! 616 # Cavium Octeon
>> 617 #
>> 618 core-$(CONFIG_CPU_CAVIUM_OCTEON) += arch/mips/cavium-octeon/
>> 619 cflags-$(CONFIG_CPU_CAVIUM_OCTEON) += -I$(srctree)/arch/mips/include/asm/mach-cavium-octeon
>> 620 core-$(CONFIG_CPU_CAVIUM_OCTEON) += arch/mips/cavium-octeon/executive/
>> 621 ifdef CONFIG_CAVIUM_OCTEON_2ND_KERNEL
>> 622 load-$(CONFIG_CPU_CAVIUM_OCTEON) += 0xffffffff84100000
190 else 623 else
191 DEFAULT_KBUILD_IMAGE = $(boot)/Image !! 624 load-$(CONFIG_CPU_CAVIUM_OCTEON) += 0xffffffff81100000
192 endif 625 endif
193 626
194 install: KBUILD_IMAGE := $(DEFAULT_KBUILD_IMAG !! 627 cflags-y += -I$(srctree)/arch/mips/include/asm/mach-generic
195 install zinstall: !! 628 drivers-$(CONFIG_PCI) += arch/mips/pci/
196 $(call cmd,install) <<
197 629
198 archprepare: !! 630 #
199 $(Q)$(MAKE) $(build)=arch/arm64/tools !! 631 # Automatically detect the build format. By default we choose
200 ifeq ($(CONFIG_ARM64_ERRATUM_843419),y) !! 632 # the elf format according to the load address.
201 ifneq ($(CONFIG_ARM64_LD_HAS_FIX_ERRATUM_843 !! 633 # We can always force a build with a 64-bits symbol format by
202 @echo "warning: ld does not support -- !! 634 # passing 'KBUILD_SYM32=no' option to the make's command line.
>> 635 #
>> 636 ifdef CONFIG_64BIT
>> 637 ifndef KBUILD_SYM32
>> 638 ifeq ($(shell expr $(load-y) \< 0xffffffff80000000), 0)
>> 639 KBUILD_SYM32 = y
>> 640 endif
203 endif 641 endif
204 endif !! 642
205 ifeq ($(CONFIG_ARM64_USE_LSE_ATOMICS),y) !! 643 ifeq ($(KBUILD_SYM32)$(call cc-option-yn,-msym32), yy)
206 ifneq ($(CONFIG_ARM64_LSE_ATOMICS),y) !! 644 cflags-y += -msym32 -DKBUILD_64BIT_SYM32
207 @echo "warning: LSE atomics not suppor !! 645 else
>> 646 ifeq ($(CONFIG_CPU_DADDI_WORKAROUNDS), y)
>> 647 $(error CONFIG_CPU_DADDI_WORKAROUNDS unsupported without -msym32)
>> 648 endif
208 endif 649 endif
209 endif 650 endif
210 651
211 ifeq ($(KBUILD_EXTMOD),) !! 652 KBUILD_AFLAGS += $(cflags-y)
212 # We need to generate vdso-offsets.h before co !! 653 KBUILD_CFLAGS += $(cflags-y)
213 # In order to do that, we should use the archp !! 654 KBUILD_CPPFLAGS += -D"VMLINUX_LOAD_ADDRESS=$(load-y)"
214 # asm-offsets.h is included in some files used !! 655 KBUILD_CPPFLAGS += -D"DATAOFFSET=$(if $(dataoffset-y),$(dataoffset-y),0)"
215 # asm-offsets.h is built in prepare0, for whic !! 656
216 # Therefore we need to generate the header aft !! 657 LDFLAGS += -m $(ld-emul)
217 # this hack. !! 658
218 prepare: vdso_prepare !! 659 ifdef CONFIG_MIPS
219 vdso_prepare: prepare0 !! 660 CHECKFLAGS += $(shell $(CC) $(KBUILD_CFLAGS) -dM -E -x c /dev/null | \
220 $(Q)$(MAKE) $(build)=arch/arm64/kernel !! 661 egrep -vw '__GNUC_(|MINOR_|PATCHLEVEL_)_' | \
221 include/generated/vdso-offsets.h arch/ !! 662 sed -e 's/^\#define /-D/' -e "s/ /='/" -e "s/$$/'/")
222 ifdef CONFIG_COMPAT_VDSO !! 663 ifdef CONFIG_64BIT
223 $(Q)$(MAKE) $(build)=arch/arm64/kernel !! 664 CHECKFLAGS += -m64
224 arch/arm64/kernel/vdso32/vdso.so <<
225 endif 665 endif
226 endif 666 endif
227 667
228 vdso-install-y += arc !! 668 OBJCOPYFLAGS += --remove-section=.reginfo
229 vdso-install-$(CONFIG_COMPAT_VDSO) += arc !! 669
230 !! 670 head-y := arch/mips/kernel/head.o arch/mips/kernel/init_task.o
231 include $(srctree)/scripts/Makefile.defconf !! 671
232 !! 672 libs-y += arch/mips/lib/
233 PHONY += virtconfig !! 673
234 virtconfig: !! 674 core-y += arch/mips/kernel/ arch/mips/mm/ arch/mips/math-emu/
235 $(call merge_into_defconfig_override,d !! 675
>> 676 drivers-$(CONFIG_OPROFILE) += arch/mips/oprofile/
>> 677
>> 678 # suspend and hibernation support
>> 679 drivers-$(CONFIG_PM) += arch/mips/power/
>> 680
>> 681 ifdef CONFIG_LASAT
>> 682 rom.bin rom.sw: vmlinux
>> 683 $(Q)$(MAKE) $(build)=arch/mips/lasat/image $@
>> 684 endif
>> 685
>> 686 #
>> 687 # Some machines like the Indy need 32-bit ELF binaries for booting purposes.
>> 688 # Other need ECOFF, so we build a 32-bit ELF binary for them which we then
>> 689 # convert to ECOFF using elf2ecoff.
>> 690 #
>> 691 vmlinux.32: vmlinux
>> 692 $(OBJCOPY) -O $(32bit-bfd) $(OBJCOPYFLAGS) $< $@
>> 693
>> 694 #
>> 695 # The 64-bit ELF tools are pretty broken so at this time we generate 64-bit
>> 696 # ELF files from 32-bit files by conversion.
>> 697 #
>> 698 vmlinux.64: vmlinux
>> 699 $(OBJCOPY) -O $(64bit-bfd) $(OBJCOPYFLAGS) $< $@
>> 700
>> 701 makeboot =$(Q)$(MAKE) $(build)=arch/mips/boot VMLINUX=$(vmlinux-32) $(1)
>> 702
>> 703 all: $(all-y)
>> 704
>> 705 vmlinux.bin: $(vmlinux-32)
>> 706 +@$(call makeboot,$@)
>> 707
>> 708 vmlinux.ecoff: $(vmlinux-32)
>> 709 +@$(call makeboot,$@)
>> 710
>> 711 vmlinux.srec: $(vmlinux-32)
>> 712 +@$(call makeboot,$@)
>> 713
>> 714 CLEAN_FILES += vmlinux.ecoff \
>> 715 vmlinux.srec
>> 716
>> 717 archprepare:
>> 718 ifdef CONFIG_MIPS32_N32
>> 719 @echo ' Checking missing-syscalls for N32'
>> 720 $(Q)$(MAKE) $(build)=. missing-syscalls EXTRA_CFLAGS="-mabi=n32"
>> 721 endif
>> 722 ifdef CONFIG_MIPS32_O32
>> 723 @echo ' Checking missing-syscalls for O32'
>> 724 $(Q)$(MAKE) $(build)=. missing-syscalls EXTRA_CFLAGS="-mabi=32"
>> 725 endif
>> 726
>> 727 install:
>> 728 $(Q)install -D -m 755 vmlinux $(INSTALL_PATH)/vmlinux-$(KERNELRELEASE)
>> 729 $(Q)install -D -m 644 .config $(INSTALL_PATH)/config-$(KERNELRELEASE)
>> 730 $(Q)install -D -m 644 System.map $(INSTALL_PATH)/System.map-$(KERNELRELEASE)
>> 731
>> 732 archclean:
>> 733 @$(MAKE) $(clean)=arch/mips/boot
>> 734 @$(MAKE) $(clean)=arch/mips/lasat
236 735
237 define archhelp 736 define archhelp
238 echo '* Image.gz - Compressed kernel i !! 737 echo ' install - install kernel into $(INSTALL_PATH)'
239 echo ' Image - Uncompressed kernel !! 738 echo ' vmlinux.ecoff - ECOFF boot image'
240 echo ' image.fit - Flat Image Tree (ar !! 739 echo ' vmlinux.bin - Raw binary boot image'
241 echo ' install - Install kernel (com !! 740 echo ' vmlinux.srec - SREC boot image'
242 echo ' zinstall - Install compressed !! 741 echo
243 echo ' Install using (your !! 742 echo ' These will be default as apropriate for a configured platform.'
244 echo ' (distribution) /sbi <<
245 echo ' install to $$(INSTA <<
246 endef 743 endef
>> 744
>> 745 CLEAN_FILES += vmlinux.32 \
>> 746 vmlinux.64 \
>> 747 vmlinux.ecoff
Linux® is a registered trademark of Linus Torvalds in the United States and other countries.
TOMOYO® is a registered trademark of NTT DATA CORPORATION.