1 // SPDX-License-Identifier: GPL-2.0-only 1
2 /*
3 * linux/lib/raid6/neon.c - RAID6 syndrome cal
4 *
5 * Copyright (C) 2013 Linaro Ltd <ard.biesheuv
6 */
7
8 #include <linux/raid/pq.h>
9
10 #ifdef __KERNEL__
11 #include <asm/neon.h>
12 #else
13 #define kernel_neon_begin()
14 #define kernel_neon_end()
15 #define cpu_has_neon() (1)
16 #endif
17
18 /*
19 * There are 2 reasons these wrappers are kept
20 * from the actual implementations in neonN.c
21 * unroll.awk):
22 * - the actual implementations use NEON intri
23 * (arm_neon.h) is not fully compatible (typ
24 * - the neonN.c files are compiled with -mfpu
25 * and we have to make sure that we never us
26 * outside a kernel_neon_begin()/kernel_neon
27 */
28
29 #define RAID6_NEON_WRAPPER(_n)
30 static void raid6_neon ## _n ## _gen_s
31 size_t
32 {
33 void raid6_neon ## _n ## _gen
34
35 kernel_neon_begin();
36 raid6_neon ## _n ## _gen_syndr
37 (unsig
38 kernel_neon_end();
39 }
40 static void raid6_neon ## _n ## _xor_s
41 int st
42 size_t
43 {
44 void raid6_neon ## _n ## _xor
45 int, int, unsi
46 kernel_neon_begin();
47 raid6_neon ## _n ## _xor_syndr
48 start, stop, (unsigned
49 kernel_neon_end();
50 }
51 struct raid6_calls const raid6_neonx #
52 raid6_neon ## _n ## _gen_syndr
53 raid6_neon ## _n ## _xor_syndr
54 raid6_have_neon,
55 "neonx" #_n,
56 0
57 }
58
59 static int raid6_have_neon(void)
60 {
61 return cpu_has_neon();
62 }
63
64 RAID6_NEON_WRAPPER(1);
65 RAID6_NEON_WRAPPER(2);
66 RAID6_NEON_WRAPPER(4);
67 RAID6_NEON_WRAPPER(8);
68
Linux® is a registered trademark of Linus Torvalds in the United States and other countries.
TOMOYO® is a registered trademark of NTT DATA CORPORATION.