1 # 1 #
2 # arch/arm/Makefile !! 2 # i386/Makefile
3 # 3 #
4 # This file is included by the global makefile 4 # This file is included by the global makefile so that you can add your own
5 # architecture-specific flags and dependencies !! 5 # architecture-specific flags and dependencies. Remember to do have actions
>> 6 # for "archclean" cleaning up for this architecture.
6 # 7 #
7 # This file is subject to the terms and condit 8 # This file is subject to the terms and conditions of the GNU General Public
8 # License. See the file "COPYING" in the main 9 # License. See the file "COPYING" in the main directory of this archive
9 # for more details. 10 # for more details.
10 # 11 #
11 # Copyright (C) 1995-2001 by Russell King !! 12 # Copyright (C) 1994 by Linus Torvalds
12 <<
13 LDFLAGS_vmlinux := --no-undefined -X --pic-ven <<
14 ifeq ($(CONFIG_CPU_ENDIAN_BE8),y) <<
15 LDFLAGS_vmlinux += --be8 <<
16 KBUILD_LDFLAGS_MODULE += --be8 <<
17 endif <<
18 <<
19 GZFLAGS :=-9 <<
20 #KBUILD_CFLAGS +=-pipe <<
21 <<
22 # Never generate .eh_frame <<
23 KBUILD_CFLAGS += $(call cc-option,-fno-dwarf <<
24 <<
25 # Disable FDPIC ABI <<
26 KBUILD_CFLAGS += $(call cc-option,-mno-fdpic <<
27 <<
28 # This should work on most of the modern platf <<
29 KBUILD_DEFCONFIG := multi_v7_defconfig <<
30 <<
31 # defines filename extension depending memory <<
32 ifeq ($(CONFIG_MMU),) <<
33 MMUEXT := -nommu <<
34 KBUILD_CFLAGS += $(call cc-option,-mno-unali <<
35 endif <<
36 <<
37 ifeq ($(CONFIG_FRAME_POINTER),y) <<
38 KBUILD_CFLAGS +=-fno-omit-frame-pointer <<
39 ifeq ($(CONFIG_CC_IS_GCC),y) <<
40 KBUILD_CFLAGS += -mapcs -mno-sched-prolog <<
41 endif <<
42 endif <<
43 <<
44 ifeq ($(CONFIG_CPU_BIG_ENDIAN),y) <<
45 KBUILD_CPPFLAGS += -mbig-endian <<
46 CHECKFLAGS += -D__ARMEB__ <<
47 KBUILD_LDFLAGS += -EB <<
48 else <<
49 KBUILD_CPPFLAGS += -mlittle-endian <<
50 CHECKFLAGS += -D__ARMEL__ <<
51 KBUILD_LDFLAGS += -EL <<
52 endif <<
53 <<
54 # 13 #
55 # The Scalar Replacement of Aggregates (SRA) o !! 14 # 19990713 Artur Skawina <skawina@geocities.com>
56 # later may result in code being generated tha !! 15 # Added '-march' and '-mpreferred-stack-boundary' support
57 # char struct members incorrectly. So disable <<
58 # (https://gcc.gnu.org/bugzilla/show_bug.cgi?i <<
59 # 16 #
60 KBUILD_CFLAGS += $(call cc-option,-fno-ipa-s <<
61 17
62 # This selects which instruction set is used. !! 18 LDFLAGS := -m elf_i386
63 arch-$(CONFIG_CPU_32v7M) :=-march=armv7 !! 19 OBJCOPYFLAGS := -O binary -R .note -R .comment -S
64 arch-$(CONFIG_CPU_32v7) :=-march=armv7 !! 20 LDFLAGS_vmlinux :=
65 arch-$(CONFIG_CPU_32v6) :=-march=armv6 !! 21
66 # Only override the compiler option if ARMv6. !! 22 CFLAGS += -pipe
67 # always available in ARMv7 !! 23
68 ifeq ($(CONFIG_CPU_32v6),y) !! 24 # prevent gcc from keeping the stack 16 byte aligned
69 arch-$(CONFIG_CPU_32v6K) :=-march=armv6 !! 25 CFLAGS += $(call check_gcc,-mpreferred-stack-boundary=2,)
70 endif !! 26
71 arch-$(CONFIG_CPU_32v5) :=-march=armv5 !! 27 align := $(subst -functions=0,,$(call check_gcc,-falign-functions=0,-malign-functions=0))
72 arch-$(CONFIG_CPU_32v4T) :=-march=armv4 !! 28
73 arch-$(CONFIG_CPU_32v4) :=-march=armv4 !! 29 cflags-$(CONFIG_M386) += -march=i386
74 arch-$(CONFIG_CPU_32v3) :=-march=armv3 !! 30 cflags-$(CONFIG_M486) += -march=i486
75 !! 31 cflags-$(CONFIG_M586) += -march=i586
76 # Note that GCC does not numerically define an !! 32 cflags-$(CONFIG_M586TSC) += -march=i586
77 # macro, but instead defines a whole series of !! 33 cflags-$(CONFIG_M586MMX) += $(call check_gcc,-march=pentium-mmx,-march=i586)
78 # testing for a specific architecture or later !! 34 cflags-$(CONFIG_M686) += -march=i686
79 cpp-$(CONFIG_CPU_32v7M) :=-D__LINUX_AR !! 35 cflags-$(CONFIG_MPENTIUMII) += $(call check_gcc,-march=pentium2,-march=i686)
80 cpp-$(CONFIG_CPU_32v7) :=-D__LINUX_AR !! 36 cflags-$(CONFIG_MPENTIUMIII) += $(call check_gcc,-march=pentium3,-march=i686)
81 cpp-$(CONFIG_CPU_32v6) :=-D__LINUX_AR !! 37 cflags-$(CONFIG_MPENTIUM4) += $(call check_gcc,-march=pentium4,-march=i686)
82 # Only override the compiler option if ARMv6. !! 38 cflags-$(CONFIG_MK6) += $(call check_gcc,-march=k6,-march=i586)
83 # always available in ARMv7 !! 39 # Please note, that patches that add -march=athlon-xp and friends are pointless.
84 ifeq ($(CONFIG_CPU_32v6),y) !! 40 # They make zero difference whatsosever to performance at this time.
85 cpp-$(CONFIG_CPU_32v6K) :=-D__LINUX_AR !! 41 cflags-$(CONFIG_MK7) += $(call check_gcc,-march=athlon,-march=i686 $(align)-functions=4)
86 endif !! 42 cflags-$(CONFIG_MK8) += $(call check_gcc,-march=k8,$(call check_gcc,-march=athlon,-march=i686 $(align)-functions=4))
87 cpp-$(CONFIG_CPU_32v5) :=-D__LINUX_AR !! 43 cflags-$(CONFIG_MCRUSOE) += -march=i686 $(align)-functions=0 $(align)-jumps=0 $(align)-loops=0
88 cpp-$(CONFIG_CPU_32v4T) :=-D__LINUX_AR !! 44 cflags-$(CONFIG_MWINCHIPC6) += $(call check_gcc,-march=winchip-c6,-march=i586)
89 cpp-$(CONFIG_CPU_32v4) :=-D__LINUX_AR !! 45 cflags-$(CONFIG_MWINCHIP2) += $(call check_gcc,-march=winchip2,-march=i586)
90 cpp-$(CONFIG_CPU_32v3) :=-D__LINUX_AR !! 46 cflags-$(CONFIG_MWINCHIP3D) += $(call check_gcc,-march=winchip2,-march=i586)
91 !! 47 cflags-$(CONFIG_MCYRIXIII) += $(call check_gcc,-march=c3,-march=i486) $(align)-functions=0 $(align)-jumps=0 $(align)-loops=0
92 # This selects how we optimise for the process !! 48 cflags-$(CONFIG_MVIAC3_2) += $(call check_gcc,-march=c3-2,-march=i686)
93 tune-$(CONFIG_CPU_ARM7TDMI) :=-mtune=arm7t !! 49
94 tune-$(CONFIG_CPU_ARM720T) :=-mtune=arm7t !! 50 CFLAGS += $(cflags-y)
95 tune-$(CONFIG_CPU_ARM740T) :=-mtune=arm7t !! 51
96 tune-$(CONFIG_CPU_ARM9TDMI) :=-mtune=arm9t !! 52 # Default subarch .c files
97 tune-$(CONFIG_CPU_ARM940T) :=-mtune=arm9t !! 53 mcore-y := mach-default
98 tune-$(CONFIG_CPU_ARM946E) :=-mtune=arm9e !! 54
99 tune-$(CONFIG_CPU_ARM920T) :=-mtune=arm9t !! 55 # Voyager subarch support
100 tune-$(CONFIG_CPU_ARM922T) :=-mtune=arm9t !! 56 mflags-$(CONFIG_X86_VOYAGER) := -Iinclude/asm-i386/mach-voyager
101 tune-$(CONFIG_CPU_ARM925T) :=-mtune=arm9t !! 57 mcore-$(CONFIG_X86_VOYAGER) := mach-voyager
102 tune-$(CONFIG_CPU_ARM926T) :=-mtune=arm9t !! 58
103 tune-$(CONFIG_CPU_FA526) :=-mtune=arm9t !! 59 # VISWS subarch support
104 tune-$(CONFIG_CPU_SA110) :=-mtune=stron !! 60 mflags-$(CONFIG_X86_VISWS) := -Iinclude/asm-i386/mach-visws
105 tune-$(CONFIG_CPU_SA1100) :=-mtune=stron !! 61 mcore-$(CONFIG_X86_VISWS) := mach-visws
106 tune-$(CONFIG_CPU_XSCALE) :=-mtune=xscal !! 62
107 tune-$(CONFIG_CPU_XSC3) :=-mtune=xscal !! 63 # NUMAQ subarch support
108 tune-$(CONFIG_CPU_FEROCEON) :=-mtune=xscal !! 64 mflags-$(CONFIG_X86_NUMAQ) := -Iinclude/asm-i386/mach-numaq
109 tune-$(CONFIG_CPU_V6) :=-mtune=arm11 !! 65 mcore-$(CONFIG_X86_NUMAQ) := mach-default
110 tune-$(CONFIG_CPU_V6K) :=-mtune=arm11 !! 66
111 !! 67 # BIGSMP subarch support
112 ifeq ($(CONFIG_AEABI),y) !! 68 mflags-$(CONFIG_X86_BIGSMP) := -Iinclude/asm-i386/mach-bigsmp
113 CFLAGS_ABI :=-mabi=aapcs-linux -mfpu=vfp !! 69 mcore-$(CONFIG_X86_BIGSMP) := mach-default
114 else !! 70
115 CFLAGS_ABI :=$(call cc-option,-mapcs-32,- !! 71 #Summit subarch support
116 endif !! 72 mflags-$(CONFIG_X86_SUMMIT) := -Iinclude/asm-i386/mach-summit
117 !! 73 mcore-$(CONFIG_X86_SUMMIT) := mach-default
118 ifeq ($(CONFIG_ARM_UNWIND),y) !! 74
119 CFLAGS_ABI +=-funwind-tables !! 75 # generic subarchitecture
120 endif !! 76 mflags-$(CONFIG_X86_GENERICARCH) := -Iinclude/asm-i386/mach-generic
121 !! 77 mcore-$(CONFIG_X86_GENERICARCH) := mach-default
122 ifeq ($(CONFIG_CC_IS_CLANG),y) !! 78 core-$(CONFIG_X86_GENERICARCH) += arch/i386/mach-generic/
123 CFLAGS_ABI += -meabi gnu !! 79
124 endif !! 80 # ES7000 subarch support
125 !! 81 mflags-$(CONFIG_X86_ES7000) := -Iinclude/asm-i386/mach-es7000
126 ifeq ($(CONFIG_CURRENT_POINTER_IN_TPIDRURO),y) !! 82 mcore-$(CONFIG_X86_ES7000) := mach-es7000
127 KBUILD_CFLAGS += -mtp=cp15 !! 83
128 endif !! 84 # default subarch .h files
129 !! 85 mflags-y += -Iinclude/asm-i386/mach-default
130 # Accept old syntax despite ".syntax unified" !! 86
131 AFLAGS_NOWARN :=$(call as-option,-Wa$(comma) !! 87 head-y := arch/i386/kernel/head.o arch/i386/kernel/init_task.o
132 !! 88
133 # The GCC option -ffreestanding is required in !! 89 libs-y += arch/i386/lib/
134 # ARM/NEON intrinsics in a non C99-compliant e !! 90 core-y += arch/i386/kernel/ \
135 CC_FLAGS_FPU := -ffreestanding !! 91 arch/i386/mm/ \
136 # Enable <arm_neon.h> !! 92 arch/i386/$(mcore-y)/
137 CC_FLAGS_FPU += -isystem $(shell $(CC) -pri !! 93 drivers-$(CONFIG_MATH_EMULATION) += arch/i386/math-emu/
138 CC_FLAGS_FPU += -march=armv7-a -mfloat-abi= !! 94 drivers-$(CONFIG_PCI) += arch/i386/pci/
139 !! 95 # must be linked after kernel/
140 ifeq ($(CONFIG_THUMB2_KERNEL),y) !! 96 drivers-$(CONFIG_OPROFILE) += arch/i386/oprofile/
141 CFLAGS_ISA :=-Wa,-mimplicit-it=always $(A !! 97 drivers-$(CONFIG_PM) += arch/i386/power/
142 AFLAGS_ISA :=$(CFLAGS_ISA) -Wa$(comma)-mt !! 98
143 CFLAGS_ISA +=-mthumb !! 99 CFLAGS += $(mflags-y)
144 else !! 100 AFLAGS += $(mflags-y)
145 CFLAGS_ISA :=$(call cc-option,-marm,) $(A !! 101
146 AFLAGS_ISA :=$(CFLAGS_ISA) !! 102 boot := arch/i386/boot
147 endif !! 103
148 !! 104 .PHONY: zImage bzImage compressed zlilo bzlilo \
149 # Need -Uarm for gcc < 3.x !! 105 zdisk bzdisk fdimage fdimage144 fdimage288 install
150 KBUILD_CPPFLAGS +=$(cpp-y) !! 106
151 KBUILD_CFLAGS +=$(CFLAGS_ABI) $(CFLAGS_ISA) !! 107 all: bzImage
152 KBUILD_AFLAGS +=$(CFLAGS_ABI) $(AFLAGS_ISA) !! 108
153 !! 109 BOOTIMAGE=arch/i386/boot/bzImage
154 CHECKFLAGS += -D__arm__ !! 110 zImage zlilo zdisk: BOOTIMAGE=arch/i386/boot/zImage
155 !! 111
156 # Text offset. This list is sorted numerically !! 112 zImage bzImage: vmlinux
157 # provide a means to avoid/resolve conflicts i !! 113 $(Q)$(MAKE) $(build)=$(boot) $(BOOTIMAGE)
158 # Note: the 32kB below this value is reserved !! 114
159 # during boot, and this offset is critical to !! 115 compressed: zImage
160 # kexec-tools. !! 116
161 textofs-y := 0x00008000 !! 117 zlilo bzlilo: vmlinux
162 # RTD1195 has Boot ROM at start of address spa !! 118 $(Q)$(MAKE) $(build)=$(boot) BOOTIMAGE=$(BOOTIMAGE) zlilo
163 textofs-$(CONFIG_ARCH_REALTEK) := 0x00108000 !! 119
164 # SA1111 DMA bug: we don't want the kernel to !! 120 zdisk bzdisk: vmlinux
165 ifeq ($(CONFIG_ARCH_SA1100),y) !! 121 $(Q)$(MAKE) $(build)=$(boot) BOOTIMAGE=$(BOOTIMAGE) zdisk
166 textofs-$(CONFIG_SA1111) := 0x00208000 !! 122
167 endif !! 123 install fdimage fdimage144 fdimage288: vmlinux
168 textofs-$(CONFIG_ARCH_QCOM_RESERVE_SMEM) := 0x !! 124 $(Q)$(MAKE) $(build)=$(boot) BOOTIMAGE=$(BOOTIMAGE) $@
169 textofs-$(CONFIG_ARCH_MESON) := 0x00208000 !! 125
170 textofs-$(CONFIG_ARCH_AXXIA) := 0x00308000 !! 126 prepare: include/asm-$(ARCH)/asm_offsets.h
171 !! 127 CLEAN_FILES += include/asm-$(ARCH)/asm_offsets.h
172 # Machine directory name. This list is sorted !! 128
173 # by CONFIG_* macro name. !! 129 arch/$(ARCH)/kernel/asm-offsets.s: include/asm include/linux/version.h \
174 machine-$(CONFIG_ARCH_ACTIONS) += act !! 130 include/config/MARKER
175 machine-$(CONFIG_ARCH_ALPINE) += alp !! 131
176 machine-$(CONFIG_ARCH_ARTPEC) += art !! 132 include/asm-$(ARCH)/asm_offsets.h: arch/$(ARCH)/kernel/asm-offsets.s
177 machine-$(CONFIG_ARCH_ASPEED) += asp !! 133 $(call filechk,gen-asm-offsets)
178 machine-$(CONFIG_ARCH_AT91) += at9 !! 134
179 machine-$(CONFIG_ARCH_AXXIA) += axx !! 135 archclean:
180 machine-$(CONFIG_ARCH_BCM) += bcm !! 136 $(Q)$(MAKE) $(clean)=arch/i386/boot
181 machine-$(CONFIG_ARCH_BERLIN) += ber <<
182 machine-$(CONFIG_ARCH_CLPS711X) += clp <<
183 machine-$(CONFIG_ARCH_DAVINCI) += dav <<
184 machine-$(CONFIG_ARCH_DIGICOLOR) += dig <<
185 machine-$(CONFIG_ARCH_DOVE) += dov <<
186 machine-$(CONFIG_ARCH_EXYNOS) += exy <<
187 machine-$(CONFIG_ARCH_FOOTBRIDGE) += foo <<
188 machine-$(CONFIG_ARCH_GEMINI) += gem <<
189 machine-$(CONFIG_ARCH_HIGHBANK) += hig <<
190 machine-$(CONFIG_ARCH_HISI) += his <<
191 machine-$(CONFIG_ARCH_HPE) += hpe <<
192 machine-$(CONFIG_ARCH_IXP4XX) += ixp <<
193 machine-$(CONFIG_ARCH_KEYSTONE) += key <<
194 machine-$(CONFIG_ARCH_LPC18XX) += lpc <<
195 machine-$(CONFIG_ARCH_LPC32XX) += lpc <<
196 machine-$(CONFIG_ARCH_MESON) += mes <<
197 machine-$(CONFIG_ARCH_MMP) += mmp <<
198 machine-$(CONFIG_ARCH_MV78XX0) += mv7 <<
199 machine-$(CONFIG_ARCH_MVEBU) += mve <<
200 machine-$(CONFIG_ARCH_MXC) += imx <<
201 machine-$(CONFIG_ARCH_MEDIATEK) += med <<
202 machine-$(CONFIG_ARCH_MILBEAUT) += mil <<
203 machine-$(CONFIG_ARCH_MXS) += mxs <<
204 machine-$(CONFIG_ARCH_MSTARV7) += mst <<
205 machine-$(CONFIG_ARCH_NOMADIK) += nom <<
206 machine-$(CONFIG_ARCH_NPCM) += npc <<
207 machine-$(CONFIG_ARCH_OMAP1) += oma <<
208 machine-$(CONFIG_ARCH_OMAP2PLUS) += oma <<
209 machine-$(CONFIG_ARCH_ORION5X) += ori <<
210 machine-$(CONFIG_ARCH_PXA) += pxa <<
211 machine-$(CONFIG_ARCH_QCOM) += qco <<
212 machine-$(CONFIG_ARCH_REALTEK) += rea <<
213 machine-$(CONFIG_ARCH_ROCKCHIP) += roc <<
214 machine-$(CONFIG_ARCH_RPC) += rpc <<
215 machine-$(CONFIG_PLAT_SAMSUNG) += s3c <<
216 machine-$(CONFIG_ARCH_S5PV210) += s5p <<
217 machine-$(CONFIG_ARCH_SA1100) += sa1 <<
218 machine-$(CONFIG_ARCH_RENESAS) += shm <<
219 machine-$(CONFIG_ARCH_INTEL_SOCFPGA) += soc <<
220 machine-$(CONFIG_ARCH_STI) += sti <<
221 machine-$(CONFIG_ARCH_STM32) += stm <<
222 machine-$(CONFIG_ARCH_SUNXI) += sun <<
223 machine-$(CONFIG_ARCH_TEGRA) += teg <<
224 machine-$(CONFIG_ARCH_U8500) += ux5 <<
225 machine-$(CONFIG_ARCH_VT8500) += vt8 <<
226 machine-$(CONFIG_ARCH_ZYNQ) += zyn <<
227 machine-$(CONFIG_PLAT_VERSATILE) += ver <<
228 machine-$(CONFIG_PLAT_SPEAR) += spe <<
229 <<
230 # legacy platforms provide their own mach/*.h <<
231 # these three are mutually exclusive <<
232 machdirs-$(CONFIG_ARCH_FOOTBRIDGE) += arc <<
233 machdirs-$(CONFIG_ARCH_RPC) += arc <<
234 machdirs-$(CONFIG_ARCH_SA1100) += arc <<
235 KBUILD_CPPFLAGS += $(patsubst %,-I$(srctree)/% <<
236 <<
237 # The byte offset of the kernel image in RAM f <<
238 TEXT_OFFSET := $(textofs-y) <<
239 <<
240 export TEXT_OFFSET GZFLAGS MMUEXT <<
241 <<
242 # If we have a machine-specific directory, the <<
243 core-y += $(patsubst <<
244 # For cleaning <<
245 core- += $(patsubst <<
246 <<
247 core-$(CONFIG_PLAT_ORION) += arch/arm/pl <<
248 <<
249 libs-y := arch/arm/li <<
250 <<
251 # Default target when executing plain make <<
252 boot := arch/arm/boot <<
253 ifeq ($(CONFIG_XIP_KERNEL),y) <<
254 KBUILD_IMAGE := $(boot)/xipImage <<
255 else <<
256 KBUILD_IMAGE := $(boot)/zImage <<
257 endif <<
258 <<
259 ifeq ($(CONFIG_STACKPROTECTOR_PER_TASK),y) <<
260 prepare: stack_protector_prepare <<
261 ifeq ($(CONFIG_CC_HAVE_STACKPROTECTOR_TLS),y) <<
262 stack_protector_prepare: prepare0 <<
263 $(eval KBUILD_CFLAGS += \ <<
264 -mstack-protector-guard=tls \ <<
265 -mstack-protector-guard-offset <<
266 awk '{if ($$2 == "TSK_ <<
267 include/genera <<
268 else <<
269 stack_protector_prepare: prepare0 <<
270 $(eval SSP_PLUGIN_CFLAGS := \ <<
271 -fplugin-arg-arm_ssp_per_task_ <<
272 awk '{if ($$2 == "TSK_ <<
273 include/genera <<
274 $(eval KBUILD_CFLAGS += $(SSP_PLUGIN_C <<
275 $(eval GCC_PLUGINS_CFLAGS += $(SSP_PLU <<
276 endif <<
277 endif <<
278 <<
279 all: $(notdir $(KBUILD_IMAGE)) <<
280 <<
281 <<
282 archheaders: <<
283 $(Q)$(MAKE) $(build)=arch/arm/tools ua <<
284 <<
285 archprepare: <<
286 $(Q)$(MAKE) $(build)=arch/arm/tools ka <<
287 <<
288 # Convert bzImage to zImage <<
289 bzImage: zImage <<
290 <<
291 BOOT_TARGETS = zImage Image xipImage bootpI <<
292 INSTALL_TARGETS = zinstall uinstall install <<
293 <<
294 PHONY += bzImage $(BOOT_TARGETS) $(INSTALL_TAR <<
295 <<
296 bootpImage uImage: zImage <<
297 zImage: Image <<
298 <<
299 $(BOOT_TARGETS): vmlinux <<
300 $(Q)$(MAKE) $(build)=$(boot) $(boot)/$ <<
301 @$(kecho) ' Kernel: $(boot)/$@ is rea <<
302 <<
303 $(INSTALL_TARGETS): KBUILD_IMAGE = $(boot)/$(p <<
304 $(INSTALL_TARGETS): <<
305 $(call cmd,install) <<
306 <<
307 vdso-install-$(CONFIG_VDSO) += arch/arm/vdso/v <<
308 <<
309 # My testing targets (bypasses dependencies) <<
310 bp:; $(Q)$(MAKE) $(build)=$(boot) $(boot)/b <<
311 <<
312 include $(srctree)/scripts/Makefile.defconf <<
313 PHONY += multi_v7_lpae_defconfig <<
314 multi_v7_lpae_defconfig: <<
315 $(call merge_into_defconfig,multi_v7_d <<
316 137
317 define archhelp 138 define archhelp
318 echo '* zImage - Compressed kernel i !! 139 echo '* bzImage - Compressed kernel image (arch/$(ARCH)/boot/bzImage)'
319 echo ' Image - Uncompressed kernel !! 140 echo ' install - Install kernel using'
320 echo '* xipImage - XIP kernel image, i !! 141 echo ' (your) ~/bin/installkernel or'
321 echo ' uImage - U-Boot wrapped zIma !! 142 echo ' (distribution) /sbin/installkernel or'
322 echo ' bootpImage - Combined zImage and !! 143 echo ' install to $$(INSTALL_PATH) and run lilo'
323 echo ' (supply initrd imag !! 144 echo ' bzdisk - Create a boot floppy in /dev/fd0'
324 echo ' install - Install uncompresse !! 145 echo ' fdimage - Create a boot floppy image'
325 echo ' zinstall - Install compressed <<
326 echo ' uinstall - Install U-Boot wrap <<
327 echo ' Install using (your <<
328 echo ' (distribution) /sbi <<
329 echo ' install to $$(INSTA <<
330 echo <<
331 echo ' multi_v7_lpae_defconfig - multi <<
332 endef 146 endef
>> 147
>> 148 CLEAN_FILES += arch/$(ARCH)/boot/fdimage arch/$(ARCH)/boot/mtools.conf
Linux® is a registered trademark of Linus Torvalds in the United States and other countries.
TOMOYO® is a registered trademark of NTT DATA CORPORATION.