Home
last modified time | relevance | path

Searched full:volatile (Results 1 – 25 of 3006) sorted by relevance

12345678910>>...121

/OK3568_Linux_fs/kernel/tools/perf/arch/x86/tests/
H A Dinsn-x86-dat-src.c21 asm volatile("rdtsc"); /* Start here */ in main()
25 asm volatile("vcvtph2ps %xmm3,%ymm5"); in main()
31 asm volatile("cmovno %rax,%rbx"); in main()
32 asm volatile("cmovno 0x12345678(%rax),%rcx"); in main()
33 asm volatile("cmovno 0x12345678(%rax),%cx"); in main()
35 asm volatile("cmove %rax,%rbx"); in main()
36 asm volatile("cmove 0x12345678(%rax),%rcx"); in main()
37 asm volatile("cmove 0x12345678(%rax),%cx"); in main()
39 asm volatile("seto 0x12345678(%rax)"); in main()
40 asm volatile("setno 0x12345678(%rax)"); in main()
[all …]
/OK3568_Linux_fs/kernel/drivers/video/fbdev/kyro/
H A DSTG4000Reg.h76 volatile u32 Thread0Enable; /* 0x0000 */
77 volatile u32 Thread1Enable; /* 0x0004 */
78 volatile u32 Thread0Recover; /* 0x0008 */
79 volatile u32 Thread1Recover; /* 0x000C */
80 volatile u32 Thread0Step; /* 0x0010 */
81 volatile u32 Thread1Step; /* 0x0014 */
82 volatile u32 VideoInStatus; /* 0x0018 */
83 volatile u32 Core2InSignStart; /* 0x001C */
84 volatile u32 Core1ResetVector; /* 0x0020 */
85 volatile u32 Core1ROMOffset; /* 0x0024 */
[all …]
/OK3568_Linux_fs/kernel/lib/raid6/
H A Dsse2.c48 asm volatile("movdqa %0,%%xmm0" : : "m" (raid6_sse_constants.x1d[0])); in raid6_sse21_gen_syndrome()
49 asm volatile("pxor %xmm5,%xmm5"); /* Zero temp */ in raid6_sse21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse21_gen_syndrome()
53 asm volatile("movdqa %0,%%xmm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse21_gen_syndrome()
54 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
55 asm volatile("movdqa %xmm2,%xmm4"); /* Q[0] */ in raid6_sse21_gen_syndrome()
56 asm volatile("movdqa %0,%%xmm6" : : "m" (dptr[z0-1][d])); in raid6_sse21_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse21_gen_syndrome()
59 asm volatile("pcmpgtb %xmm4,%xmm5"); in raid6_sse21_gen_syndrome()
60 asm volatile("paddb %xmm4,%xmm4"); in raid6_sse21_gen_syndrome()
[all …]
H A Davx2.c46 asm volatile("vmovdqa %0,%%ymm0" : : "m" (raid6_avx2_constants.x1d[0])); in raid6_avx21_gen_syndrome()
47 asm volatile("vpxor %ymm3,%ymm3,%ymm3"); /* Zero temp */ in raid6_avx21_gen_syndrome()
50 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_avx21_gen_syndrome()
51 asm volatile("vmovdqa %0,%%ymm2" : : "m" (dptr[z0][d]));/* P[0] */ in raid6_avx21_gen_syndrome()
52 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
53 asm volatile("vmovdqa %ymm2,%ymm4");/* Q[0] */ in raid6_avx21_gen_syndrome()
54 asm volatile("vmovdqa %0,%%ymm6" : : "m" (dptr[z0-1][d])); in raid6_avx21_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_avx21_gen_syndrome()
57 asm volatile("vpcmpgtb %ymm4,%ymm3,%ymm5"); in raid6_avx21_gen_syndrome()
58 asm volatile("vpaddb %ymm4,%ymm4,%ymm4"); in raid6_avx21_gen_syndrome()
[all …]
H A Drecov_ssse3.c54 asm volatile("movdqa %0,%%xmm7" : : "m" (x0f[0])); in raid6_2data_recov_ssse3()
57 asm volatile("movdqa %0,%%xmm6" : : "m" (qmul[0])); in raid6_2data_recov_ssse3()
58 asm volatile("movdqa %0,%%xmm14" : : "m" (pbmul[0])); in raid6_2data_recov_ssse3()
59 asm volatile("movdqa %0,%%xmm15" : : "m" (pbmul[16])); in raid6_2data_recov_ssse3()
67 asm volatile("movdqa %0,%%xmm1" : : "m" (q[0])); in raid6_2data_recov_ssse3()
68 asm volatile("movdqa %0,%%xmm9" : : "m" (q[16])); in raid6_2data_recov_ssse3()
69 asm volatile("movdqa %0,%%xmm0" : : "m" (p[0])); in raid6_2data_recov_ssse3()
70 asm volatile("movdqa %0,%%xmm8" : : "m" (p[16])); in raid6_2data_recov_ssse3()
71 asm volatile("pxor %0,%%xmm1" : : "m" (dq[0])); in raid6_2data_recov_ssse3()
72 asm volatile("pxor %0,%%xmm9" : : "m" (dq[16])); in raid6_2data_recov_ssse3()
[all …]
H A Drecov_avx2.c53 asm volatile("vpbroadcastb %0, %%ymm7" : : "m" (x0f)); in raid6_2data_recov_avx2()
57 asm volatile("vmovdqa %0, %%ymm1" : : "m" (q[0])); in raid6_2data_recov_avx2()
58 asm volatile("vmovdqa %0, %%ymm9" : : "m" (q[32])); in raid6_2data_recov_avx2()
59 asm volatile("vmovdqa %0, %%ymm0" : : "m" (p[0])); in raid6_2data_recov_avx2()
60 asm volatile("vmovdqa %0, %%ymm8" : : "m" (p[32])); in raid6_2data_recov_avx2()
61 asm volatile("vpxor %0, %%ymm1, %%ymm1" : : "m" (dq[0])); in raid6_2data_recov_avx2()
62 asm volatile("vpxor %0, %%ymm9, %%ymm9" : : "m" (dq[32])); in raid6_2data_recov_avx2()
63 asm volatile("vpxor %0, %%ymm0, %%ymm0" : : "m" (dp[0])); in raid6_2data_recov_avx2()
64 asm volatile("vpxor %0, %%ymm8, %%ymm8" : : "m" (dp[32])); in raid6_2data_recov_avx2()
73 asm volatile("vbroadcasti128 %0, %%ymm4" : : "m" (qmul[0])); in raid6_2data_recov_avx2()
[all …]
H A Dsse1.c52 asm volatile("movq %0,%%mm0" : : "m" (raid6_mmx_constants.x1d)); in raid6_sse11_gen_syndrome()
53 asm volatile("pxor %mm5,%mm5"); /* Zero temp */ in raid6_sse11_gen_syndrome()
56 asm volatile("prefetchnta %0" : : "m" (dptr[z0][d])); in raid6_sse11_gen_syndrome()
57 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_sse11_gen_syndrome()
58 asm volatile("prefetchnta %0" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
59 asm volatile("movq %mm2,%mm4"); /* Q[0] */ in raid6_sse11_gen_syndrome()
60 asm volatile("movq %0,%%mm6" : : "m" (dptr[z0-1][d])); in raid6_sse11_gen_syndrome()
62 asm volatile("prefetchnta %0" : : "m" (dptr[z][d])); in raid6_sse11_gen_syndrome()
63 asm volatile("pcmpgtb %mm4,%mm5"); in raid6_sse11_gen_syndrome()
64 asm volatile("paddb %mm4,%mm4"); in raid6_sse11_gen_syndrome()
[all …]
H A Dmmx.c47 asm volatile("movq %0,%%mm0" : : "m" (raid6_mmx_constants.x1d)); in raid6_mmx1_gen_syndrome()
48 asm volatile("pxor %mm5,%mm5"); /* Zero temp */ in raid6_mmx1_gen_syndrome()
51 asm volatile("movq %0,%%mm2" : : "m" (dptr[z0][d])); /* P[0] */ in raid6_mmx1_gen_syndrome()
52 asm volatile("movq %mm2,%mm4"); /* Q[0] */ in raid6_mmx1_gen_syndrome()
54 asm volatile("movq %0,%%mm6" : : "m" (dptr[z][d])); in raid6_mmx1_gen_syndrome()
55 asm volatile("pcmpgtb %mm4,%mm5"); in raid6_mmx1_gen_syndrome()
56 asm volatile("paddb %mm4,%mm4"); in raid6_mmx1_gen_syndrome()
57 asm volatile("pand %mm0,%mm5"); in raid6_mmx1_gen_syndrome()
58 asm volatile("pxor %mm5,%mm4"); in raid6_mmx1_gen_syndrome()
59 asm volatile("pxor %mm5,%mm5"); in raid6_mmx1_gen_syndrome()
[all …]
/OK3568_Linux_fs/kernel/arch/arm/mach-iop32x/
H A Diop3xx.h56 #define IOP3XX_ATUVID (volatile u16 *)IOP3XX_REG_ADDR(0x0100)
57 #define IOP3XX_ATUDID (volatile u16 *)IOP3XX_REG_ADDR(0x0102)
58 #define IOP3XX_ATUCMD (volatile u16 *)IOP3XX_REG_ADDR(0x0104)
59 #define IOP3XX_ATUSR (volatile u16 *)IOP3XX_REG_ADDR(0x0106)
60 #define IOP3XX_ATURID (volatile u8 *)IOP3XX_REG_ADDR(0x0108)
61 #define IOP3XX_ATUCCR (volatile u32 *)IOP3XX_REG_ADDR(0x0109)
62 #define IOP3XX_ATUCLSR (volatile u8 *)IOP3XX_REG_ADDR(0x010c)
63 #define IOP3XX_ATULT (volatile u8 *)IOP3XX_REG_ADDR(0x010d)
64 #define IOP3XX_ATUHTR (volatile u8 *)IOP3XX_REG_ADDR(0x010e)
65 #define IOP3XX_ATUBIST (volatile u8 *)IOP3XX_REG_ADDR(0x010f)
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-aarch64/include/opencv2/core/cuda/
H A Dreduce.hpp63 __device__ __forceinline__ void reduce(volatile T* smem, T& val, unsigned int tid, const Op& op) in reduce()
65 …reduce_detail::Dispatcher<N>::reductor::template reduce<volatile T*, T&, const Op&>(smem, val, tid… in reduce()
83 …__device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, volatile V* svals, V& val,… in reduceKeyVal()
85 …reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, volatile V*, V&, … in reduceKeyVal()
92 __device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, in reduceKeyVal()
97 reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, in reduceKeyVal()
128 thrust::tuple<volatile T0*>
131 return thrust::make_tuple((volatile T0*) t0); in smem_tuple()
136 thrust::tuple<volatile T0*, volatile T1*>
139 return thrust::make_tuple((volatile T0*) t0, (volatile T1*) t1); in smem_tuple()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/OpenCV-android-sdk/sdk/native/jni/include/opencv2/core/cuda/
H A Dreduce.hpp63 __device__ __forceinline__ void reduce(volatile T* smem, T& val, unsigned int tid, const Op& op) in reduce()
65 …reduce_detail::Dispatcher<N>::reductor::template reduce<volatile T*, T&, const Op&>(smem, val, tid… in reduce()
83 …__device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, volatile V* svals, V& val,… in reduceKeyVal()
85 …reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, volatile V*, V&, … in reduceKeyVal()
92 __device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, in reduceKeyVal()
97 reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, in reduceKeyVal()
128 thrust::tuple<volatile T0*>
131 return thrust::make_tuple((volatile T0*) t0); in smem_tuple()
136 thrust::tuple<volatile T0*, volatile T1*>
139 return thrust::make_tuple((volatile T0*) t0, (volatile T1*) t1); in smem_tuple()
[all …]
/OK3568_Linux_fs/external/rknpu2/examples/3rdparty/opencv/opencv-linux-armhf/include/opencv2/core/cuda/
H A Dreduce.hpp63 __device__ __forceinline__ void reduce(volatile T* smem, T& val, unsigned int tid, const Op& op) in reduce()
65 …reduce_detail::Dispatcher<N>::reductor::template reduce<volatile T*, T&, const Op&>(smem, val, tid… in reduce()
83 …__device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, volatile V* svals, V& val,… in reduceKeyVal()
85 …reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, volatile V*, V&, … in reduceKeyVal()
92 __device__ __forceinline__ void reduceKeyVal(volatile K* skeys, K& key, in reduceKeyVal()
97 reduce_key_val_detail::Dispatcher<N>::reductor::template reduce<volatile K*, K&, in reduceKeyVal()
128 thrust::tuple<volatile T0*>
131 return thrust::make_tuple((volatile T0*) t0); in smem_tuple()
136 thrust::tuple<volatile T0*, volatile T1*>
139 return thrust::make_tuple((volatile T0*) t0, (volatile T1*) t1); in smem_tuple()
[all …]
/OK3568_Linux_fs/kernel/arch/mips/include/asm/txx9/
H A Dtx3927.h26 volatile unsigned long cr[8];
27 volatile unsigned long tr[3];
28 volatile unsigned long cmd;
29 volatile unsigned long smrs[2];
33 volatile unsigned long cr[8];
38 volatile unsigned long cha;
39 volatile unsigned long sar;
40 volatile unsigned long dar;
41 volatile unsigned long cntr;
42 volatile unsigned long sair;
[all …]
/OK3568_Linux_fs/kernel/arch/m68k/include/asm/
H A Dmvme147hw.h23 #define m147_rtc ((MK48T02 * volatile)0xfffe07f8)
27 volatile u_long dma_tadr;
28 volatile u_long dma_dadr;
29 volatile u_long dma_bcr;
30 volatile u_long dma_hr;
31 volatile u_short t1_preload;
32 volatile u_short t1_count;
33 volatile u_short t2_preload;
34 volatile u_short t2_count;
35 volatile u_char t1_int_cntrl;
[all …]
/OK3568_Linux_fs/kernel/arch/mips/include/asm/ip32/
H A Dmace.h24 volatile unsigned int error_addr;
25 volatile unsigned int error;
49 volatile unsigned int control;
70 volatile unsigned int rev;
72 volatile unsigned int config_addr;
74 volatile unsigned char b[4];
75 volatile unsigned short w[2];
76 volatile unsigned int l;
98 volatile u64 mac_ctrl;
99 volatile unsigned long int_stat;
[all …]
/OK3568_Linux_fs/kernel/arch/ia64/include/uapi/asm/
H A Dgcc_intrin.h17 /* The "volatile" is due to gcc bugs */
18 #define ia64_barrier() asm volatile ("":::"memory")
20 #define ia64_stop() asm volatile (";;"::)
22 #define ia64_invala_gr(regnum) asm volatile ("invala.e r%0" :: "i"(regnum))
24 #define ia64_invala_fr(regnum) asm volatile ("invala.e f%0" :: "i"(regnum))
26 #define ia64_flushrs() asm volatile ("flushrs;;":::"memory")
28 #define ia64_loadrs() asm volatile ("loadrs;;":::"memory")
38 asm volatile ("mov psr.l=%0" :: "r"(val) : "memory"); \
41 asm volatile ("mov ar%0=%1" :: \
46 asm volatile ("mov cr%0=%1" :: \
[all …]
/OK3568_Linux_fs/buildroot/dl/qt5location/git/src/3rdparty/mapbox-gl-native/deps/boost/1.65.1/include/boost/type_traits/detail/
H A Dis_mem_fun_pointer_tester.hpp46 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)());
49 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)() const);
52 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)() volatile);
55 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)() const volatile);
58 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)( ...));
61 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)( ...) const);
64 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)( ...) volatile);
67 yes_type is_mem_fun_pointer_tester(R (T::*const volatile*)( ...) const volatile);
70 yes_type is_mem_fun_pointer_tester(R (__stdcall T::*const volatile*)());
73 yes_type is_mem_fun_pointer_tester(R (__stdcall T::*const volatile*)() const);
[all …]
/OK3568_Linux_fs/kernel/include/video/
H A Dgbe.h12 volatile uint32_t ctrlstat; /* general control */
13 volatile uint32_t dotclock; /* dot clock PLL control */
14 volatile uint32_t i2c; /* crt I2C control */
15 volatile uint32_t sysclk; /* system clock PLL control */
16 volatile uint32_t i2cfp; /* flat panel I2C control */
17 volatile uint32_t id; /* device id/chip revision */
18 volatile uint32_t config; /* power on configuration [1] */
19 volatile uint32_t bist; /* internal bist status [1] */
21 volatile uint32_t vt_xy; /* current dot coords */
22 volatile uint32_t vt_xymax; /* maximum dot coords */
[all …]
/OK3568_Linux_fs/kernel/arch/parisc/include/asm/
H A Dhardware.h43 volatile uint32_t nothing; /* reg 0 */
44 volatile uint32_t io_eim;
45 volatile uint32_t io_dc_adata;
46 volatile uint32_t io_ii_cdata;
47 volatile uint32_t io_dma_link; /* reg 4 */
48 volatile uint32_t io_dma_command;
49 volatile uint32_t io_dma_address;
50 volatile uint32_t io_dma_count;
51 volatile uint32_t io_flex; /* reg 8 */
52 volatile uint32_t io_spa_address;
[all …]
/OK3568_Linux_fs/external/security/rk_tee_user/v2/export-ta_arm32/include/libcxx/include/
H A Datomic55 bool test_and_set(memory_order m = memory_order_seq_cst) volatile noexcept;
57 void clear(memory_order m = memory_order_seq_cst) volatile noexcept;
62 atomic_flag& operator=(const atomic_flag&) volatile = delete;
66 atomic_flag_test_and_set(volatile atomic_flag* obj) noexcept;
72 atomic_flag_test_and_set_explicit(volatile atomic_flag* obj,
79 atomic_flag_clear(volatile atomic_flag* obj) noexcept;
85 atomic_flag_clear_explicit(volatile atomic_flag* obj, memory_order m) noexcept;
97 bool is_lock_free() const volatile noexcept;
99 void store(T desr, memory_order m = memory_order_seq_cst) volatile noexcept;
101 T load(memory_order m = memory_order_seq_cst) const volatile noexcept;
[all …]
/OK3568_Linux_fs/external/security/rk_tee_user/v2/export-ta_arm64/include/libcxx/include/
H A Datomic55 bool test_and_set(memory_order m = memory_order_seq_cst) volatile noexcept;
57 void clear(memory_order m = memory_order_seq_cst) volatile noexcept;
62 atomic_flag& operator=(const atomic_flag&) volatile = delete;
66 atomic_flag_test_and_set(volatile atomic_flag* obj) noexcept;
72 atomic_flag_test_and_set_explicit(volatile atomic_flag* obj,
79 atomic_flag_clear(volatile atomic_flag* obj) noexcept;
85 atomic_flag_clear_explicit(volatile atomic_flag* obj, memory_order m) noexcept;
97 bool is_lock_free() const volatile noexcept;
99 void store(T desr, memory_order m = memory_order_seq_cst) volatile noexcept;
101 T load(memory_order m = memory_order_seq_cst) const volatile noexcept;
[all …]
/OK3568_Linux_fs/kernel/arch/mips/include/asm/sgi/
H A Dmc.h18 volatile u32 cpuctrl0; /* CPU control register 0, readwrite */
39 volatile u32 cpuctrl1; /* CPU control register 1, readwrite */
49 volatile u32 watchdogt; /* Watchdog reg rdonly, write clears */
52 volatile u32 systemid; /* MC system ID register, readonly */
57 volatile u32 divider; /* Divider reg for RPSS */
68 volatile u32 rcntpre; /* Preload refresh counter */
71 volatile u32 rcounter; /* Readonly refresh counter */
74 volatile u32 giopar; /* Parameter word for GIO64 */
93 volatile u32 cputp; /* CPU bus arb time period */
96 volatile u32 lbursttp; /* Time period for long bursts */
[all …]
/OK3568_Linux_fs/kernel/arch/alpha/include/asm/
H A Dio_trivial.h12 return __kernel_ldbu(*(const volatile u8 __force *)a); in IO_CONCAT()
18 return __kernel_ldwu(*(const volatile u16 __force *)a); in IO_CONCAT()
24 __kernel_stb(b, *(volatile u8 __force *)a); in IO_CONCAT()
30 __kernel_stw(b, *(volatile u16 __force *)a); in IO_CONCAT()
38 return *(const volatile u32 __force *)a; in IO_CONCAT()
44 *(volatile u32 __force *)a = b; in IO_CONCAT()
50 IO_CONCAT(__IO_PREFIX,readb)(const volatile void __iomem *a) in IO_CONCAT()
52 return __kernel_ldbu(*(const volatile u8 __force *)a); in IO_CONCAT()
56 IO_CONCAT(__IO_PREFIX,readw)(const volatile void __iomem *a) in IO_CONCAT()
58 return __kernel_ldwu(*(const volatile u16 __force *)a); in IO_CONCAT()
[all …]
H A Dio.h63 static inline unsigned long virt_to_phys(volatile void *address) in virt_to_phys()
73 static inline unsigned long virt_to_phys(volatile void *address) in virt_to_phys()
109 static inline unsigned long __deprecated virt_to_bus(volatile void *address) in virt_to_bus()
156 REMAP1(u8, readb, const volatile) in REMAP1()
157 REMAP1(u16, readw, const volatile) in REMAP1()
158 REMAP1(u32, readl, const volatile) in REMAP1()
159 REMAP1(u64, readq, const volatile) in REMAP1()
164 REMAP2(u8, writeb, volatile) in REMAP1()
165 REMAP2(u16, writew, volatile) in REMAP1()
166 REMAP2(u32, writel, volatile) in REMAP1()
[all …]
/OK3568_Linux_fs/kernel/arch/powerpc/kernel/
H A Dio.c27 void _insb(const volatile u8 __iomem *port, void *buf, long count) in _insb()
34 asm volatile("sync"); in _insb()
40 asm volatile("twi 0,%0,0; isync" : : "r" (tmp)); in _insb()
44 void _outsb(volatile u8 __iomem *port, const void *buf, long count) in _outsb()
50 asm volatile("sync"); in _outsb()
54 asm volatile("sync"); in _outsb()
58 void _insw_ns(const volatile u16 __iomem *port, void *buf, long count) in _insw_ns()
65 asm volatile("sync"); in _insw_ns()
71 asm volatile("twi 0,%0,0; isync" : : "r" (tmp)); in _insw_ns()
75 void _outsw_ns(volatile u16 __iomem *port, const void *buf, long count) in _outsw_ns()
[all …]

12345678910>>...121