Searched refs:__always_inline (Results 276 - 300 of 730) sorted by relevance

<<11121314151617181920>>

/linux-master/include/linux/sched/
H A Dtopology.h266 static __always_inline
274 static __always_inline
282 static __always_inline
289 static __always_inline
/linux-master/tools/testing/selftests/bpf/progs/
H A Dxdping_kern.c28 static __always_inline void swap_src_dst_mac(void *data)
44 static __always_inline __u16 csum_fold_helper(__wsum sum)
50 static __always_inline __u16 ipv4_csum(void *data_start, int data_size)
60 static __always_inline int icmp_check(struct xdp_md *ctx, int type)
H A Dxdp_synproxy_kern.c112 static __always_inline void swap_eth_addr(__u8 *a, __u8 *b)
121 static __always_inline __u16 csum_fold(__u32 csum)
128 static __always_inline __u16 csum_tcpudp_magic(__be32 saddr, __be32 daddr,
149 static __always_inline __u16 csum_ipv6_magic(const struct in6_addr *saddr,
174 static __always_inline __u64 tcp_clock_ns(void)
179 static __always_inline __u32 tcp_ns_to_ts(__u64 ns)
184 static __always_inline __u32 tcp_clock_ms(void)
199 static __always_inline u8 *next(struct tcpopt_context *ctx, __u32 sz)
274 static __always_inline bool tscookie_init(struct tcphdr *tcp_header,
310 static __always_inline voi
[all...]
H A Dtest_xdp.c38 static __always_inline void count_tx(__u32 protocol)
47 static __always_inline int get_dport(void *trans_data, void *data_end,
69 static __always_inline void set_ethhdr(struct ethhdr *new_eth,
79 static __always_inline int handle_ipv4(struct xdp_md *xdp)
152 static __always_inline int handle_ipv6(struct xdp_md *xdp)
/linux-master/arch/x86/include/asm/
H A Dbarrier.h36 static __always_inline unsigned long array_index_mask_nospec(unsigned long index,
/linux-master/kernel/
H A Dstackleak.c74 static __always_inline void __stackleak_poison(unsigned long erase_low,
85 static __always_inline void __stackleak_erase(bool on_task_stack)
H A Dcontext_tracking.c42 static __always_inline void rcu_dynticks_task_enter(void)
50 static __always_inline void rcu_dynticks_task_exit(void)
58 static __always_inline void rcu_dynticks_task_trace_enter(void)
67 static __always_inline void rcu_dynticks_task_trace_exit(void)
426 static __always_inline void ct_kernel_exit(bool user, int offset) { }
427 static __always_inline void ct_kernel_enter(bool user, int offset) { }
452 static __always_inline void context_tracking_recursion_exit(void)
/linux-master/arch/riscv/include/asm/
H A Dswitch_to.h60 static __always_inline bool has_fpu(void)
66 static __always_inline bool has_fpu(void) { return false; }
H A Dvector.h38 static __always_inline bool has_vector(void)
68 static __always_inline void riscv_v_enable(void)
73 static __always_inline void riscv_v_disable(void)
78 static __always_inline void __vstate_csr_save(struct __riscv_v_ext_state *dest)
90 static __always_inline void __vstate_csr_restore(struct __riscv_v_ext_state *src)
270 static __always_inline bool has_vector(void) { return false; }
/linux-master/arch/powerpc/include/asm/
H A Dreg_fsl_emb.h14 static __always_inline unsigned int mfpmr(unsigned int rn)
27 static __always_inline void mtpmr(unsigned int rn, unsigned int val)
H A Dinterrupt.h424 static __always_inline __no_sanitize_address __no_kcsan long \
439 static __always_inline __no_sanitize_address __no_kcsan long \
459 static __always_inline void ____##func(struct pt_regs *regs); \
471 static __always_inline void ____##func(struct pt_regs *regs)
492 static __always_inline long ____##func(struct pt_regs *regs); \
508 static __always_inline long ____##func(struct pt_regs *regs)
527 static __always_inline void ____##func(struct pt_regs *regs); \
539 static __always_inline void ____##func(struct pt_regs *regs)
560 static __always_inline __no_sanitize_address __no_kcsan long \
578 static __always_inline __no_sanitize_addres
[all...]
/linux-master/fs/bcachefs/
H A Dstr_hash.h162 static __always_inline int
192 static __always_inline int
205 static __always_inline int
231 static __always_inline
261 static __always_inline
323 static __always_inline
339 static __always_inline
365 static __always_inline
H A Dbkey.h103 static __always_inline bool bpos_eq(struct bpos l, struct bpos r)
110 static __always_inline bool bpos_lt(struct bpos l, struct bpos r)
117 static __always_inline bool bpos_le(struct bpos l, struct bpos r)
124 static __always_inline bool bpos_gt(struct bpos l, struct bpos r)
129 static __always_inline bool bpos_ge(struct bpos l, struct bpos r)
134 static __always_inline int bpos_cmp(struct bpos l, struct bpos r)
151 static __always_inline bool bkey_eq(struct bpos l, struct bpos r)
157 static __always_inline bool bkey_lt(struct bpos l, struct bpos r)
164 static __always_inline bool bkey_le(struct bpos l, struct bpos r)
171 static __always_inline boo
[all...]
/linux-master/tools/include/linux/
H A Drbtree.h177 static __always_inline void
205 static __always_inline void
233 static __always_inline struct rb_node *
266 static __always_inline struct rb_node *
294 static __always_inline struct rb_node *
324 static __always_inline struct rb_node *
/linux-master/include/linux/
H A Drbtree.h164 static __always_inline struct rb_node *
194 static __always_inline void
222 static __always_inline struct rb_node *
255 static __always_inline struct rb_node *
283 static __always_inline struct rb_node *
313 static __always_inline struct rb_node *
H A Dbitops.h94 static __always_inline unsigned long hweight_long(unsigned long w)
186 static __always_inline __s32 sign_extend32(__u32 value, int index)
197 static __always_inline __s64 sign_extend64(__u64 value, int index)
275 static __always_inline void assign_bit(long nr, volatile unsigned long *addr,
284 static __always_inline void __assign_bit(long nr, volatile unsigned long *addr,
H A Dthread_info.h122 * This may be used in noinstr code, and needs to be __always_inline to prevent
125 static __always_inline unsigned long read_ti_thread_flags(struct thread_info *ti)
182 static __always_inline bool tif_need_resched(void)
190 static __always_inline bool tif_need_resched(void)
211 static __always_inline void check_object_size(const void *ptr, unsigned long n,
236 static __always_inline __must_check bool
/linux-master/include/uapi/linux/
H A Dswab.h136 static __always_inline unsigned long __swab(const unsigned long y)
171 static __always_inline __u16 __swab16p(const __u16 *p)
184 static __always_inline __u32 __swab32p(const __u32 *p)
197 static __always_inline __u64 __swab64p(const __u64 *p)
252 static __always_inline void __swab32s(__u32 *p)
265 static __always_inline void __swab64s(__u64 *p)
/linux-master/arch/alpha/include/asm/
H A Dbitops.h49 static __always_inline void
85 static __always_inline void
121 static __always_inline void
189 static __always_inline bool
233 static __always_inline bool
275 static __always_inline bool
/linux-master/arch/arm64/include/asm/
H A Dinsn.h296 static __always_inline bool aarch64_insn_is_##abbr(u32 code) \
301 static __always_inline u32 aarch64_insn_get_##abbr##_value(void) \
431 static __always_inline bool aarch64_insn_is_steppable_hint(u32 insn)
455 static __always_inline bool aarch64_insn_is_branch(u32 insn)
474 static __always_inline bool aarch64_insn_is_branch_imm(u32 insn)
485 static __always_inline bool aarch64_insn_is_adr_adrp(u32 insn)
491 static __always_inline bool aarch64_insn_is_dsb(u32 insn)
497 static __always_inline bool aarch64_insn_is_barrier(u32 insn)
508 static __always_inline bool aarch64_insn_is_store_single(u32 insn)
515 static __always_inline boo
[all...]
/linux-master/lib/vdso/
H A Dgettimeofday.c13 static __always_inline
21 static __always_inline u64 vdso_shift_ns(u64 ns, u32 shift)
49 static __always_inline int do_hres_timens(const struct vdso_data *vdns, clockid_t clk,
97 static __always_inline
103 static __always_inline int do_hres_timens(const struct vdso_data *vdns, clockid_t clk,
110 static __always_inline int do_hres(const struct vdso_data *vd, clockid_t clk,
165 static __always_inline int do_coarse_timens(const struct vdso_data *vdns, clockid_t clk,
194 static __always_inline int do_coarse_timens(const struct vdso_data *vdns, clockid_t clk,
201 static __always_inline int do_coarse(const struct vdso_data *vd, clockid_t clk,
227 static __always_inline in
[all...]
/linux-master/tools/testing/selftests/rseq/
H A Drseq-riscv-bits.h8 static inline __always_inline
61 static inline __always_inline
118 static inline __always_inline
162 static inline __always_inline
231 static inline __always_inline
280 static inline __always_inline
343 static inline __always_inline
/linux-master/samples/bpf/
H A Dxdp_tx_iptunnel_kern.c36 static __always_inline void count_tx(u32 protocol)
45 static __always_inline int get_dport(void *trans_data, void *data_end,
67 static __always_inline void set_ethhdr(struct ethhdr *new_eth,
77 static __always_inline int handle_ipv4(struct xdp_md *xdp)
152 static __always_inline int handle_ipv6(struct xdp_md *xdp)
/linux-master/arch/x86/kvm/
H A Dkvm_cache_regs.h19 static __always_inline unsigned long kvm_##lname##_read(struct kvm_vcpu *vcpu)\
23 static __always_inline void kvm_##lname##_write(struct kvm_vcpu *vcpu, \
84 static __always_inline bool kvm_register_test_and_mark_available(struct kvm_vcpu *vcpu,
160 static __always_inline bool kvm_is_cr0_bit_set(struct kvm_vcpu *vcpu,
182 static __always_inline bool kvm_is_cr4_bit_set(struct kvm_vcpu *vcpu,
/linux-master/drivers/gpu/drm/imagination/
H A Dpvr_fw.h462 static __always_inline void *
468 static __always_inline void
476 static __always_inline void
495 static __always_inline int
503 static __always_inline void

Completed in 221 milliseconds

<<11121314151617181920>>