| # SPDX-License-Identifier: GPL-2.0 |
| lib-y := clear_user.o delay.o copy_from_user.o \ |
| copy_to_user.o copy_page.o \ |
| clear_page.o csum.o insn.o memchr.o memcpy.o \ |
| memset.o memcmp.o strcmp.o strncmp.o strlen.o \ |
| strnlen.o strchr.o strrchr.o tishift.o |
| |
| ifeq ($(CONFIG_KERNEL_MODE_NEON), y) |
| obj-$(CONFIG_XOR_BLOCKS) += xor-neon.o |
| CFLAGS_REMOVE_xor-neon.o += -mgeneral-regs-only |
| CFLAGS_xor-neon.o += -ffreestanding |
| # Enable <arm_neon.h> |
| CFLAGS_xor-neon.o += -isystem $(shell $(CC) -print-file-name=include) |
| endif |
| |
| lib-$(CONFIG_ARCH_HAS_UACCESS_FLUSHCACHE) += uaccess_flushcache.o |
| |
| obj-$(CONFIG_CRC32) += crc32.o |
| |
| obj-$(CONFIG_FUNCTION_ERROR_INJECTION) += error-inject.o |
| |
| obj-$(CONFIG_ARM64_MTE) += mte.o |
| |
| obj-$(CONFIG_KASAN_SW_TAGS) += kasan_sw_tags.o |
