Home
last modified time | relevance | path

Searched refs:msk (Results 1 – 25 of 100) sorted by relevance

1234

/linux/tools/testing/selftests/powerpc/primitives/asm/
H A Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
63 FTR_ENTRY_LONG msk; \
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
81 #define END_FTR_SECTION(msk, val) \ argument
82 END_FTR_SECTION_NESTED(msk, val, 97)
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
85 END_FTR_SECTION_NESTED((msk), (msk), label)
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO argument
88 END_FTR_SECTION_IFCLR(msk) global() argument
92 ALT_FTR_SECTION_END_NESTED(msk,val,label) global() argument
94 ALT_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
96 ALT_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
98 ALT_FTR_SECTION_END(msk,val) global() argument
100 ALT_FTR_SECTION_END_IFSET(msk) global() argument
102 ALT_FTR_SECTION_END_IFCLR(msk) global() argument
109 END_MMU_FTR_SECTION_NESTED(msk,val,label) global() argument
113 END_MMU_FTR_SECTION(msk,val) global() argument
116 END_MMU_FTR_SECTION_NESTED_IFSET(msk,label) global() argument
119 END_MMU_FTR_SECTION_NESTED_IFCLR(msk,label) global() argument
122 END_MMU_FTR_SECTION_IFSET(msk) global() argument
123 END_MMU_FTR_SECTION_IFCLR(msk) global() argument
128 ALT_MMU_FTR_SECTION_END_NESTED(msk,val,label) global() argument
130 ALT_MMU_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
132 ALT_MMU_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
134 ALT_MMU_FTR_SECTION_END(msk,val) global() argument
136 ALT_MMU_FTR_SECTION_END_IFSET(msk) global() argument
138 ALT_MMU_FTR_SECTION_END_IFCLR(msk) global() argument
145 END_FW_FTR_SECTION_NESTED(msk,val,label) global() argument
149 END_FW_FTR_SECTION(msk,val) global() argument
152 END_FW_FTR_SECTION_IFSET(msk) global() argument
153 END_FW_FTR_SECTION_IFCLR(msk) global() argument
158 ALT_FW_FTR_SECTION_END_NESTED(msk,val,label) global() argument
160 ALT_FW_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
162 ALT_FW_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
164 ALT_FW_FTR_SECTION_END(msk,val) global() argument
166 ALT_FW_FTR_SECTION_END_IFSET(msk) global() argument
168 ALT_FW_FTR_SECTION_END_IFCLR(msk) global() argument
173 ASM_FTR_IF(section_if,section_else,msk,val) global() argument
180 ASM_FTR_IFSET(section_if,section_else,msk) global() argument
183 ASM_FTR_IFCLR(section_if,section_else,msk) global() argument
186 ASM_MMU_FTR_IF(section_if,section_else,msk,val) global() argument
193 ASM_MMU_FTR_IFSET(section_if,section_else,msk) global() argument
196 ASM_MMU_FTR_IFCLR(section_if,section_else,msk) global() argument
[all...]
/linux/arch/powerpc/include/asm/
H A Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
63 FTR_ENTRY_LONG msk; \
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
81 #define END_FTR_SECTION(msk, val) \ argument
82 END_FTR_SECTION_NESTED(msk, val, 97)
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
85 END_FTR_SECTION_NESTED((msk), (msk), label)
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
88 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
[all …]
/linux/net/mptcp/
H A Dpm.c108 static bool mptcp_pm_is_init_remote_addr(struct mptcp_sock *msk, in mptcp_pm_is_init_remote_addr() argument
113 mptcp_remote_address((struct sock_common *)msk, &mpc_remote); in mptcp_pm_is_init_remote_addr()
136 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, in mptcp_lookup_anno_list_by_saddr() argument
141 lockdep_assert_held(&msk->pm.lock); in mptcp_lookup_anno_list_by_saddr()
143 list_for_each_entry(entry, &msk->pm.anno_list, list) { in mptcp_lookup_anno_list_by_saddr()
151 bool mptcp_remove_anno_list_by_saddr(struct mptcp_sock *msk, in mptcp_remove_anno_list_by_saddr() argument
157 entry = mptcp_pm_del_add_timer(msk, addr, false); in mptcp_remove_anno_list_by_saddr()
164 bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk) in mptcp_pm_sport_in_anno_list() argument
172 spin_lock_bh(&msk->pm.lock); in mptcp_pm_sport_in_anno_list()
173 list_for_each_entry(entry, &msk in mptcp_pm_sport_in_anno_list()
185 __mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) __mptcp_pm_send_ack() argument
206 mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) mptcp_pm_send_ack() argument
215 mptcp_pm_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_addr_send_ack() argument
242 mptcp_pm_mp_prio_send_ack(struct mptcp_sock * msk,struct mptcp_addr_info * addr,struct mptcp_addr_info * rem,u8 bkup) mptcp_pm_mp_prio_send_ack() argument
272 mptcp_adjust_add_addr_timeout(struct mptcp_sock * msk) mptcp_adjust_add_addr_timeout() argument
297 struct mptcp_sock *msk = entry->sock; mptcp_pm_add_timer() local
344 mptcp_pm_del_add_timer(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool check_id) mptcp_pm_del_add_timer() argument
373 mptcp_pm_alloc_anno_list(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_alloc_anno_list() argument
410 mptcp_pm_free_anno_list(struct mptcp_sock * msk) mptcp_pm_free_anno_list() argument
430 mptcp_pm_announce_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool echo) mptcp_pm_announce_addr() argument
458 mptcp_pm_remove_addr(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_remove_addr() argument
479 mptcp_pm_new_connection(struct mptcp_sock * msk,const struct sock * ssk,int server_side) mptcp_pm_new_connection() argument
489 mptcp_pm_allow_new_subflow(struct mptcp_sock * msk) mptcp_pm_allow_new_subflow() argument
529 mptcp_pm_schedule_work(struct mptcp_sock * msk,enum mptcp_pm_status new_status) mptcp_pm_schedule_work() argument
542 mptcp_pm_fully_established(struct mptcp_sock * msk,const struct sock * ssk) mptcp_pm_fully_established() argument
569 mptcp_pm_connection_closed(struct mptcp_sock * msk) mptcp_pm_connection_closed() argument
577 mptcp_pm_subflow_established(struct mptcp_sock * msk) mptcp_pm_subflow_established() argument
594 mptcp_pm_subflow_check_next(struct mptcp_sock * msk,const struct mptcp_subflow_context * subflow) mptcp_pm_subflow_check_next() argument
630 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_add_addr_received() local
664 mptcp_pm_add_addr_echoed(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_add_addr_echoed() argument
682 mptcp_pm_add_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_add_addr_send_ack() argument
690 mptcp_pm_rm_addr_or_subflow(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list,enum linux_mptcp_mib_field rm_type) mptcp_pm_rm_addr_or_subflow() argument
753 mptcp_pm_rm_addr_recv(struct mptcp_sock * msk) mptcp_pm_rm_addr_recv() argument
758 mptcp_pm_rm_subflow(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_subflow() argument
764 mptcp_pm_rm_addr_received(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_received() argument
787 struct mptcp_sock *msk; mptcp_pm_mp_prio_received() local
800 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_mp_fail_received() local
825 mptcp_pm_add_addr_signal(struct mptcp_sock * msk,const struct sk_buff * skb,unsigned int opt_size,unsigned int remaining,struct mptcp_addr_info * addr,bool * echo,bool * drop_other_suboptions) mptcp_pm_add_addr_signal() argument
872 mptcp_pm_rm_addr_signal(struct mptcp_sock * msk,unsigned int remaining,struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_signal() argument
902 mptcp_pm_get_local_id(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_get_local_id() argument
926 mptcp_pm_is_backup(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_is_backup() argument
938 mptcp_pm_subflows_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflows_chk_stale() argument
975 mptcp_pm_subflow_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflow_chk_stale() argument
994 mptcp_pm_worker(struct mptcp_sock * msk) mptcp_pm_worker() argument
1019 mptcp_pm_destroy(struct mptcp_sock * msk) mptcp_pm_destroy() argument
1027 mptcp_pm_data_reset(struct mptcp_sock * msk) mptcp_pm_data_reset() argument
1056 mptcp_pm_data_init(struct mptcp_sock * msk) mptcp_pm_data_init() argument
[all...]
H A Dpm_kernel.c40 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk() argument
42 return pm_nl_get_pernet(sock_net((struct sock *)msk)); in pm_nl_get_pernet_from_msk()
50 u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_signal_max() argument
52 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_signal_max()
58 u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_subflow_max() argument
60 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_subflow_max()
66 u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_laminar_max() argument
68 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_laminar_max()
74 u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_fullmesh_max() argument
76 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_fullmesh_max()
[all …]
H A Dsched.c19 static int mptcp_sched_default_get_send(struct mptcp_sock *msk) in mptcp_sched_default_get_send() argument
23 ssk = mptcp_subflow_get_send(msk); in mptcp_sched_default_get_send()
31 static int mptcp_sched_default_get_retrans(struct mptcp_sock *msk)
35 ssk = mptcp_subflow_get_retrans(msk); in mptcp_sched_default_get_retrans()
130 int mptcp_init_sched(struct mptcp_sock *msk, in mptcp_init_sched()
139 msk->sched = sched; in mptcp_release_sched()
140 if (msk->sched->init) in mptcp_release_sched()
141 msk->sched->init(msk); in mptcp_release_sched()
143 pr_debug("sched=%s\n", msk in mptcp_release_sched()
32 mptcp_sched_default_get_retrans(struct mptcp_sock * msk,struct mptcp_sched_data * data) mptcp_sched_default_get_retrans() argument
119 mptcp_init_sched(struct mptcp_sock * msk,struct mptcp_sched_ops * sched) mptcp_init_sched() argument
137 mptcp_release_sched(struct mptcp_sock * msk) mptcp_release_sched() argument
157 mptcp_sched_get_send(struct mptcp_sock * msk) mptcp_sched_get_send() argument
185 mptcp_sched_get_retrans(struct mptcp_sock * msk) mptcp_sched_get_retrans() argument
[all...]
H A Dprotocol.c36 struct mptcp_sock msk; member
57 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) in mptcp_wnd_end() argument
59 return READ_ONCE(msk->wnd_end); in mptcp_wnd_end()
74 bool __mptcp_try_fallback(struct mptcp_sock *msk, int fb_mib) in __mptcp_try_fallback() argument
76 struct net *net = sock_net((struct sock *)msk); in __mptcp_try_fallback()
78 if (__mptcp_check_fallback(msk)) in __mptcp_try_fallback()
85 if (!RB_EMPTY_ROOT(&msk->out_of_order_queue)) in __mptcp_try_fallback()
88 spin_lock_bh(&msk->fallback_lock); in __mptcp_try_fallback()
89 if (!msk->allow_infinite_fallback) { in __mptcp_try_fallback()
90 spin_unlock_bh(&msk->fallback_lock); in __mptcp_try_fallback()
[all …]
H A Dsockopt.c20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback() argument
22 msk_owned_by_me(msk); in __mptcp_tcp_fallback()
24 if (likely(!__mptcp_check_fallback(msk))) in __mptcp_tcp_fallback()
27 return msk->first; in __mptcp_tcp_fallback()
42 * Needs sync from mptcp join logic, but ssk->seq == msk->seq in sockopt_seq_reset()
44 * Set High order bits to sk_state so ssk->seq == msk->seq test in sockopt_seq_reset()
51 static void sockopt_seq_inc(struct mptcp_sock *msk) in sockopt_seq_inc() argument
53 u32 seq = (msk->setsockopt_seq + 1) & 0x00ffffff; in sockopt_seq_inc()
55 msk->setsockopt_seq = sockopt_seq_reset((struct sock *)msk) in sockopt_seq_inc()
58 mptcp_get_int_option(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen,int * val) mptcp_get_int_option() argument
70 mptcp_sol_socket_sync_intval(struct mptcp_sock * msk,int optname,int val) mptcp_sol_socket_sync_intval() argument
123 mptcp_sol_socket_intval(struct mptcp_sock * msk,int optname,int val) mptcp_sol_socket_intval() argument
138 mptcp_so_incoming_cpu(struct mptcp_sock * msk,int val) mptcp_so_incoming_cpu() argument
147 mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock * msk,int optname,int val) mptcp_setsockopt_sol_socket_tstamp() argument
172 mptcp_setsockopt_sol_socket_int(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_int() argument
205 mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_timestamping() argument
249 mptcp_setsockopt_sol_socket_linger(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_linger() argument
290 mptcp_setsockopt_sol_socket(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket() argument
387 mptcp_setsockopt_v6(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v6() argument
582 mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_tcp_congestion() argument
625 __mptcp_setsockopt_set_val(struct mptcp_sock * msk,int max,int (* set_val)(struct sock *,int),int * msk_val,int val) __mptcp_setsockopt_set_val() argument
650 __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock * msk,int val) __mptcp_setsockopt_sol_tcp_cork() argument
670 __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock * msk,int val) __mptcp_setsockopt_sol_tcp_nodelay() argument
689 mptcp_setsockopt_sol_ip_set(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_ip_set() argument
735 mptcp_setsockopt_v4_set_tos(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v4_set_tos() argument
763 mptcp_setsockopt_v4(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v4() argument
779 mptcp_setsockopt_first_sf_only(struct mptcp_sock * msk,int level,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_first_sf_only() argument
801 mptcp_setsockopt_all_sf(struct mptcp_sock * msk,int level,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_all_sf() argument
818 mptcp_setsockopt_sol_tcp(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_tcp() argument
895 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_setsockopt() local
930 mptcp_getsockopt_first_sf_only(struct mptcp_sock * msk,int level,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_first_sf_only() argument
956 mptcp_diag_fill_info(struct mptcp_sock * msk,struct mptcp_info * info) mptcp_diag_fill_info() argument
1017 mptcp_getsockopt_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_info() argument
1101 mptcp_getsockopt_tcpinfo(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_tcpinfo() argument
1193 mptcp_getsockopt_subflow_addrs(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_subflow_addrs() argument
1291 mptcp_getsockopt_full_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_full_info() argument
1365 mptcp_put_int_option(struct mptcp_sock * msk,char __user * optval,int __user * optlen,int val) mptcp_put_int_option() argument
1394 mptcp_getsockopt_sol_tcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_tcp() argument
1440 mptcp_getsockopt_v4(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v4() argument
1465 mptcp_getsockopt_v6(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v6() argument
1485 mptcp_getsockopt_sol_mptcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_mptcp() argument
1505 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_getsockopt() local
1533 sync_socket_options(struct mptcp_sock * msk,struct sock * ssk) sync_socket_options() argument
1589 mptcp_sockopt_sync_locked(struct mptcp_sock * msk,struct sock * ssk) mptcp_sockopt_sync_locked() argument
[all...]
H A Dprotocol.h378 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me() argument
380 sock_owned_by_me((const struct sock *)msk); in msk_owned_by_me()
420 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head() local
422 return msk->first_pending; in mptcp_send_head()
427 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next() local
430 cur = msk->first_pending; in mptcp_send_next()
431 return list_is_last(&cur->list, &msk->rtx_queue) ? NULL : in mptcp_send_next()
437 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail() local
439 if (!msk->first_pending) in mptcp_pending_tail()
442 if (WARN_ON_ONCE(list_empty(&msk->rtx_queue))) in mptcp_pending_tail()
[all …]
H A Dtoken_test.c54 struct mptcp_sock *msk; in build_msk() local
57 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); in build_msk()
58 KUNIT_EXPECT_NOT_ERR_OR_NULL(test, msk); in build_msk()
59 refcount_set(&((struct sock *)msk)->sk_refcnt, 1); in build_msk()
60 sock_net_set((struct sock *)msk, &init_net); in build_msk()
62 sk = (struct sock *)msk; in build_msk()
68 return msk; in build_msk()
75 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
80 ctx->conn = (struct sock *)msk; in mptcp_token_test_msk_basic()
81 sk = (struct sock *)msk; in mptcp_token_test_msk_basic()
[all …]
H A Dsubflow.c44 if (subflow_req->msk) in subflow_req_destructor()
45 sock_put((struct sock *)subflow_req->msk); in subflow_req_destructor()
61 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow() argument
63 return mptcp_is_fully_established((void *)msk) && in mptcp_can_accept_new_subflow()
64 ((mptcp_pm_is_userspace(msk) && in mptcp_can_accept_new_subflow()
65 mptcp_userspace_pm_active(msk)) || in mptcp_can_accept_new_subflow()
66 READ_ONCE(msk->pm.accept_subflow)); in mptcp_can_accept_new_subflow()
72 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac() local
77 subflow_generate_hmac(READ_ONCE(msk->local_key), in subflow_req_create_thmac()
78 READ_ONCE(msk->remote_key), in subflow_req_create_thmac()
[all …]
H A Dtoken.c154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
175 WRITE_ONCE(msk->token, subflow->token); in mptcp_token_new_connect()
176 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_new_connect()
192 struct mptcp_sock *msk) in mptcp_token_accept() argument
195 struct sock *sk = (struct sock *)msk; in mptcp_token_accept()
206 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_accept()
214 struct mptcp_sock *msk; in mptcp_token_exists() local
222 msk = mptcp_sk(sk); in mptcp_token_exists()
223 if (READ_ONCE(msk->token) == token) in mptcp_token_exists()
250 struct mptcp_sock *msk; in mptcp_token_get_sock() local
[all …]
H A Doptions.c455 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp() local
487 opts->csum_reqd = READ_ONCE(msk->csum_enabled); in mptcp_established_options_mp()
568 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
575 opts->csum_reqd = READ_ONCE(msk->csum_enabled); in mptcp_established_options_dss()
599 if (!READ_ONCE(msk->can_ack)) { in mptcp_established_options_dss()
604 ack_seq = READ_ONCE(msk->ack_seq); in mptcp_established_options_dss()
605 if (READ_ONCE(msk->use_64bit_ack)) { in mptcp_established_options_dss()
660 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
670 if (!mptcp_pm_should_add_signal(msk) || in mptcp_established_options_add_addr()
672 !mptcp_pm_add_addr_signal(msk, skb, opt_size, remaining, &addr, in mptcp_established_options_add_addr()
[all …]
H A Dpm_netlink.c291 bool mptcp_userspace_pm_active(const struct mptcp_sock *msk) in mptcp_userspace_pm_active()
294 sock_net((const struct sock *)msk), in mptcp_userspace_pm_active()
346 const struct mptcp_sock *msk, in mptcp_event_put_token_and_ssk()
349 const struct sock *sk = (const struct sock *)msk; in mptcp_event_put_token_and_ssk()
353 if (nla_put_u32(skb, MPTCP_ATTR_TOKEN, READ_ONCE(msk->token))) in mptcp_event_put_token_and_ssk()
379 const struct mptcp_sock *msk, in mptcp_event_sub_established()
382 return mptcp_event_put_token_and_ssk(skb, msk, ssk); in mptcp_event_sub_established()
386 const struct mptcp_sock *msk, in mptcp_event_sub_closed()
391 if (mptcp_event_put_token_and_ssk(skb, msk, ssk)) in mptcp_event_sub_closed()
408 const struct mptcp_sock *msk, in mptcp_event_created()
290 mptcp_userspace_pm_active(const struct mptcp_sock * msk) mptcp_userspace_pm_active() argument
345 mptcp_event_put_token_and_ssk(struct sk_buff * skb,const struct mptcp_sock * msk,const struct sock * ssk) mptcp_event_put_token_and_ssk() argument
378 mptcp_event_sub_established(struct sk_buff * skb,const struct mptcp_sock * msk,const struct sock * ssk) mptcp_event_sub_established() argument
385 mptcp_event_sub_closed(struct sk_buff * skb,const struct mptcp_sock * msk,const struct sock * ssk) mptcp_event_sub_closed() argument
407 mptcp_event_created(struct sk_buff * skb,const struct mptcp_sock * msk,const struct sock * ssk) mptcp_event_created() argument
433 mptcp_event_addr_removed(const struct mptcp_sock * msk,uint8_t id) mptcp_event_addr_removed() argument
468 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_event_addr_announced() local
571 mptcp_event(enum mptcp_event_type type,const struct mptcp_sock * msk,const struct sock * ssk,gfp_t gfp) mptcp_event() argument
[all...]
H A Dsyncookies.c97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state() local
111 msk = mptcp_token_get_sock(net, e->token); in mptcp_token_join_cookie_init_state()
112 if (!msk) { in mptcp_token_join_cookie_init_state()
122 subflow_req->msk = msk; in mptcp_token_join_cookie_init_state()
/linux/drivers/net/ethernet/netronome/nfp/flower/
H A Dmatch.c12 struct nfp_flower_meta_tci *msk, u8 key_type) in nfp_flower_compile_meta() argument
18 msk->nfp_flow_key_layer = key_type; in nfp_flower_compile_meta()
19 msk->mask_id = ~0; in nfp_flower_compile_meta()
24 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_tci() argument
47 msk->tci |= cpu_to_be16(msk_tci); in nfp_flower_compile_tci()
53 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci() argument
57 memset(msk, 0, sizeof(struct nfp_flower_meta_tci)); in nfp_flower_compile_meta_tci()
59 nfp_flower_compile_meta(ext, msk, key_type); in nfp_flower_compile_meta_tci()
62 nfp_flower_compile_tci(ext, msk, rule); in nfp_flower_compile_meta_tci()
96 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mac() argument
[all …]
H A Dmain.h557 struct nfp_flower_meta_tci *msk, u8 key_type);
560 struct nfp_flower_meta_tci *msk,
570 struct nfp_flower_mac_mpls *msk,
574 struct nfp_flower_mac_mpls *msk,
579 struct nfp_flower_tp_ports *msk,
583 struct nfp_flower_vlan *msk,
587 struct nfp_flower_ipv4 *msk, struct flow_rule *rule);
590 struct nfp_flower_ipv6 *msk, struct flow_rule *rule);
592 nfp_flower_compile_geneve_opt(u8 *ext, u8 *msk, struct flow_rule *rule);
595 struct nfp_flower_ipv4_gre_tun *msk,
[all …]
/linux/net/mctp/
H A Daf_mctp.c55 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_bind() local
56 struct net *net = sock_net(&msk->sk); in mctp_bind()
82 msk->bind_local_addr = smctp->smctp_addr.s_addr; in mctp_bind()
90 msk->bind_local_addr != MCTP_ADDR_ANY) { in mctp_bind()
91 msk->bind_net = mctp_default_net(net); in mctp_bind()
93 msk->bind_net = smctp->smctp_network; in mctp_bind()
99 if (msk->bind_peer_set) { in mctp_bind()
100 if (msk->bind_type != smctp->smctp_type) { in mctp_bind()
106 if (msk->bind_net == MCTP_NET_ANY) { in mctp_bind()
108 msk in mctp_bind()
135 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_connect() local
194 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sendmsg() local
288 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_recvmsg() local
389 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_setsockopt() local
410 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_getsockopt() local
502 mctp_ioctl_alloctag(struct mctp_sock * msk,bool tagv2,unsigned long arg) mctp_ioctl_alloctag() argument
545 mctp_ioctl_droptag(struct mctp_sock * msk,bool tagv2,unsigned long arg) mctp_ioctl_droptag() argument
594 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_ioctl() local
653 struct mctp_sock *msk = container_of(timer, struct mctp_sock, mctp_sk_expire_keys() local
695 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sk_init() local
712 struct mctp_sock *msk; mctp_sk_hash() local
757 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sk_unhash() local
[all...]
H A Droute.c57 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_lookup_bind_details() local
59 if (!allow_net_any && msk->bind_net == MCTP_NET_ANY) in mctp_lookup_bind_details()
62 if (msk->bind_net != MCTP_NET_ANY && msk->bind_net != cb->net) in mctp_lookup_bind_details()
65 if (msk->bind_type != type) in mctp_lookup_bind_details()
68 if (msk->bind_peer_set && in mctp_lookup_bind_details()
69 !mctp_address_matches(msk->bind_peer_addr, src)) in mctp_lookup_bind_details()
72 if (!mctp_address_matches(msk->bind_local_addr, dest)) in mctp_lookup_bind_details()
75 return msk; in mctp_lookup_bind_details()
83 struct mctp_sock *msk; in mctp_lookup_bind() local
105 msk = mctp_lookup_bind_details(net, skb, type, mh->dest, mh->src, in mctp_lookup_bind()
[all …]
/linux/tools/testing/selftests/bpf/progs/
H A Dmptcp_sock.c32 struct mptcp_sock *msk; in _sockops() local
60 msk = bpf_skc_to_mptcp_sock(sk); in _sockops()
61 if (!msk) in _sockops()
64 storage = bpf_sk_storage_get(&socket_storage_map, msk, 0, in _sockops()
69 storage->token = msk->token; in _sockops()
70 __builtin_memcpy(storage->ca_name, msk->ca_name, TCP_CA_NAME_MAX); in _sockops()
71 storage->first = msk->first; in _sockops()
81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk, in BPF_PROG() argument
85 token = msk->token; in BPF_PROG()
/linux/kernel/irq/
H A Dmatrix.c136 const struct cpumask *msk) in matrix_find_best_cpu() argument
143 for_each_cpu(cpu, msk) { in matrix_find_best_cpu()
157 const struct cpumask *msk) in matrix_find_best_cpu_managed() argument
164 for_each_cpu(cpu, msk) { in matrix_find_best_cpu_managed()
216 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_reserve_managed() argument
220 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
237 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
257 void irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_remove_managed() argument
261 for_each_cpu(cpu, msk) { in irq_matrix_remove_managed()
292 int irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc_managed() argument
[all …]
/linux/drivers/usb/mtu3/
H A Dmtu3_host.c70 u32 reg, msk, val; in ssusb_wakeup_ip_sleep_set() local
75 msk = WC1_IS_EN | WC1_IS_C(0xf) | WC1_IS_P; in ssusb_wakeup_ip_sleep_set()
80 msk = WC0_IS_EN | WC0_IS_C(0xf) | WC0_IS_P; in ssusb_wakeup_ip_sleep_set()
85 msk = WC0_SSUSB0_CDEN | WC0_IS_SPM_EN; in ssusb_wakeup_ip_sleep_set()
86 val = enable ? msk : 0; in ssusb_wakeup_ip_sleep_set()
90 msk = WC1_IS_EN_P0_95 | WC1_IS_C_95(0xf) | WC1_IS_P_95; in ssusb_wakeup_ip_sleep_set()
95 msk = WC0_IS_EN_P2_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95; in ssusb_wakeup_ip_sleep_set()
100 msk = WC0_IS_EN_P3_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95; in ssusb_wakeup_ip_sleep_set()
105 msk = SSC_IP_SLEEP_EN | SSC_SPM_INT_EN; in ssusb_wakeup_ip_sleep_set()
106 val = enable ? msk : 0; in ssusb_wakeup_ip_sleep_set()
[all …]
/linux/drivers/clk/sprd/
H A Dpll.c54 u32 msk, u32 val) in sprd_pll_write() argument
66 regmap_write(common->regmap, offset, (reg & ~msk) | val); in sprd_pll_write()
173 cfg[index].msk = mask; in _sprd_pll_set_rate()
184 cfg[index].msk |= mask; in _sprd_pll_set_rate()
189 cfg[index].msk |= mask; in _sprd_pll_set_rate()
196 cfg[index].msk |= mask; in _sprd_pll_set_rate()
206 cfg[index].msk |= mask; in _sprd_pll_set_rate()
214 cfg[index].msk |= mask; in _sprd_pll_set_rate()
217 if (cfg[i].msk) { in _sprd_pll_set_rate()
218 sprd_pll_write(pll, i, cfg[i].msk, cfg[i].val); in _sprd_pll_set_rate()
[all …]
/linux/drivers/media/usb/pvrusb2/
H A Dpvrusb2-ctrl.c207 int msk; in pvr2_ctrl_get_valname() local
210 for (idx = 0, msk = 1; val; idx++, msk <<= 1) { in pvr2_ctrl_get_valname()
211 if (val & msk) { in pvr2_ctrl_get_valname()
291 static unsigned int gen_bitmask_string(int msk,int val,int msk_only, in gen_bitmask_string() argument
304 for (idx = 0, sm = 1; msk; idx++, sm <<= 1) { in gen_bitmask_string()
305 if (sm & msk) { in gen_bitmask_string()
306 msk &= ~sm; in gen_bitmask_string()
380 int msk; in parse_mtoken() local
382 for (idx = 0, msk = 1; valid_bits; idx++, msk <<= 1) { in parse_mtoken()
383 if (!(msk & valid_bits)) continue; in parse_mtoken()
[all …]
/linux/lib/vdso/
H A Dgettimeofday.c292 u32 msk; in __cvdso_clock_gettime_common() local
301 msk = 1U << clock; in __cvdso_clock_gettime_common()
302 if (likely(msk & VDSO_HRES)) in __cvdso_clock_gettime_common()
304 else if (msk & VDSO_COARSE) in __cvdso_clock_gettime_common()
306 else if (msk & VDSO_RAW) in __cvdso_clock_gettime_common()
308 else if (msk & VDSO_AUX) in __cvdso_clock_gettime_common()
429 u32 msk; in __cvdso_clock_getres_common() local
443 msk = 1U << clock; in __cvdso_clock_getres_common()
444 if (msk & (VDSO_HRES | VDSO_RAW)) { in __cvdso_clock_getres_common()
449 } else if (msk & VDSO_COARSE) { in __cvdso_clock_getres_common()
[all …]
/linux/drivers/net/ethernet/aquantia/atlantic/
H A Daq_hw_utils.c20 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit() argument
23 if (msk ^ ~0) { in aq_hw_write_reg_bit()
27 reg_new = (reg_old & (~msk)) | (val << shift); in aq_hw_write_reg_bit()
36 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) in aq_hw_read_reg_bit() argument
38 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift); in aq_hw_read_reg_bit()

1234