Searched refs:msk (Results 1 - 25 of 133) sorted by relevance

123456

/linux-master/arch/powerpc/include/asm/
H A Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \
63 FTR_ENTRY_LONG msk; \
77 #define END_FTR_SECTION_NESTED(msk, val, label) \
79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
81 #define END_FTR_SECTION(msk, val) \
82 END_FTR_SECTION_NESTED(msk, val, 97)
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \
85 END_FTR_SECTION_NESTED((msk), (msk), label)
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO
[all...]
/linux-master/tools/testing/selftests/powerpc/primitives/asm/
H A Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \
63 FTR_ENTRY_LONG msk; \
77 #define END_FTR_SECTION_NESTED(msk, val, label) \
79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
81 #define END_FTR_SECTION(msk, val) \
82 END_FTR_SECTION_NESTED(msk, val, 97)
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \
85 END_FTR_SECTION_NESTED((msk), (msk), label)
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO
[all...]
/linux-master/net/mptcp/
H A Dsched.c19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk, argument
24 ssk = data->reinject ? mptcp_subflow_get_retrans(msk) :
25 mptcp_subflow_get_send(msk);
108 int mptcp_init_sched(struct mptcp_sock *msk, argument
117 msk->sched = sched;
118 if (msk->sched->init)
119 msk->sched->init(msk);
121 pr_debug("sched=%s", msk->sched->name);
126 void mptcp_release_sched(struct mptcp_sock *msk) argument
146 mptcp_sched_get_send(struct mptcp_sock *msk) argument
175 mptcp_sched_get_retrans(struct mptcp_sock *msk) argument
[all...]
H A Dpm.c16 int mptcp_pm_announce_addr(struct mptcp_sock *msk, argument
20 u8 add_addr = READ_ONCE(msk->pm.addr_signal);
22 pr_debug("msk=%p, local_id=%d, echo=%d", msk, addr->id, echo);
24 lockdep_assert_held(&msk->pm.lock);
28 MPTCP_INC_STATS(sock_net((struct sock *)msk),
34 msk->pm.remote = *addr;
37 msk->pm.local = *addr;
40 WRITE_ONCE(msk->pm.addr_signal, add_addr);
44 int mptcp_pm_remove_addr(struct mptcp_sock *msk, cons argument
63 mptcp_pm_remove_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument
75 mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side) argument
85 mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) argument
124 mptcp_pm_schedule_work(struct mptcp_sock *msk, enum mptcp_pm_status new_status) argument
137 mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk) argument
164 mptcp_pm_connection_closed(struct mptcp_sock *msk) argument
169 mptcp_pm_subflow_established(struct mptcp_sock *msk) argument
186 mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct mptcp_subflow_context *subflow) argument
222 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
251 mptcp_pm_add_addr_echoed(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument
266 mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk) argument
274 mptcp_pm_rm_addr_received(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument
297 struct mptcp_sock *msk; local
310 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
331 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) argument
378 mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining, struct mptcp_rm_list *rm_list) argument
408 mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) argument
429 mptcp_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument
466 mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk) argument
510 mptcp_pm_data_reset(struct mptcp_sock *msk) argument
549 mptcp_pm_data_init(struct mptcp_sock *msk) argument
[all...]
H A Dtoken_test.c54 struct mptcp_sock *msk; local
57 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER);
58 KUNIT_EXPECT_NOT_ERR_OR_NULL(test, msk);
59 refcount_set(&((struct sock *)msk)->sk_refcnt, 1);
60 sock_net_set((struct sock *)msk, &init_net);
62 sk = (struct sock *)msk;
68 return msk;
75 struct mptcp_sock *msk = build_msk(test); local
80 ctx->conn = (struct sock *)msk;
81 sk = (struct sock *)msk;
97 struct mptcp_sock *msk = build_msk(test); local
116 struct mptcp_sock *msk = build_msk(test); local
[all...]
H A Dsockopt.c20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) argument
22 msk_owned_by_me(msk);
24 if (likely(!__mptcp_check_fallback(msk)))
27 return msk->first;
42 * Needs sync from mptcp join logic, but ssk->seq == msk->seq
44 * Set High order bits to sk_state so ssk->seq == msk->seq test
51 static void sockopt_seq_inc(struct mptcp_sock *msk) argument
53 u32 seq = (msk->setsockopt_seq + 1) & 0x00ffffff;
55 msk->setsockopt_seq = sockopt_seq_reset((struct sock *)msk)
58 mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen, int *val) argument
70 mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) argument
123 mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) argument
138 mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) argument
147 mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) argument
172 mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
205 mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
249 mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen) argument
290 mptcp_setsockopt_sol_socket(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
387 mptcp_setsockopt_v6(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
582 mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen) argument
625 __mptcp_setsockopt_set_val(struct mptcp_sock *msk, int max, int (*set_val)(struct sock *, int), int *msk_val, int val) argument
650 __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock *msk, int val) argument
670 __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock *msk, int val) argument
689 mptcp_setsockopt_sol_ip_set(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
735 mptcp_setsockopt_v4_set_tos(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
763 mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
779 mptcp_setsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname, sockptr_t optval, unsigned int optlen) argument
801 mptcp_setsockopt_sol_tcp(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument
873 struct mptcp_sock *msk = mptcp_sk(sk); local
908 mptcp_getsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname, char __user *optval, int __user *optlen) argument
935 mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info) argument
994 mptcp_getsockopt_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument
1078 mptcp_getsockopt_tcpinfo(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument
1170 mptcp_getsockopt_subflow_addrs(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument
1268 mptcp_getsockopt_full_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument
1342 mptcp_put_int_option(struct mptcp_sock *msk, char __user *optval, int __user *optlen, int val) argument
1371 mptcp_getsockopt_sol_tcp(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument
1414 mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument
1433 mptcp_getsockopt_sol_mptcp(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument
1453 struct mptcp_sock *msk = mptcp_sk(sk); local
1479 sync_socket_options(struct mptcp_sock *msk, struct sock *ssk) argument
1535 mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk) argument
[all...]
H A Dprotocol.c34 struct mptcp_sock msk; member in struct:mptcp6_sock
53 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) argument
55 return READ_ONCE(msk->wnd_end);
68 static int __mptcp_socket_create(struct mptcp_sock *msk) argument
71 struct sock *sk = (struct sock *)msk;
79 msk->scaling_ratio = tcp_sk(ssock->sk)->scaling_ratio;
80 WRITE_ONCE(msk->first, ssock->sk);
82 list_add(&subflow->node, &msk->conn_list);
85 subflow->subflow_id = msk->subflow_id++;
89 mptcp_sock_graft(msk
98 __mptcp_nmpc_sk(struct mptcp_sock *msk) argument
158 mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, struct sk_buff *from) argument
176 struct mptcp_sock *msk = mptcp_sk(sk); local
209 mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) argument
322 struct mptcp_sock *msk = mptcp_sk(sk); local
338 __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, struct sk_buff *skb, unsigned int offset, size_t copy_len) argument
416 struct mptcp_sock *msk = mptcp_sk(sk); local
425 struct mptcp_sock *msk = mptcp_sk(sk); local
448 struct mptcp_sock *msk = mptcp_sk(sk); local
521 mptcp_send_ack(struct mptcp_sock *msk) argument
552 mptcp_cleanup_rbuf(struct mptcp_sock *msk) argument
573 struct mptcp_sock *msk = mptcp_sk(sk); local
621 __mptcp_move_skbs_from_subflow(struct mptcp_sock *msk, struct sock *ssk, unsigned int *bytes) argument
716 __mptcp_ofo_queue(struct mptcp_sock *msk) argument
794 struct mptcp_sock *msk = mptcp_sk(sk); local
804 move_skbs_to_msk(struct mptcp_sock *msk, struct sock *ssk) argument
831 struct mptcp_sock *msk = mptcp_sk(sk); local
859 mptcp_subflow_joined(struct mptcp_sock *msk, struct sock *ssk) argument
866 __mptcp_finish_join(struct mptcp_sock *msk, struct sock *ssk) argument
890 struct mptcp_sock *msk = mptcp_sk(sk); local
934 mptcp_subflow_recv_lookup(const struct mptcp_sock *msk) argument
967 mptcp_frag_can_collapse_to(const struct mptcp_sock *msk, const struct page_frag *pfrag, const struct mptcp_data_frag *df) argument
995 struct mptcp_sock *msk = mptcp_sk(sk); local
1070 struct mptcp_sock *msk = mptcp_sk(sk); local
1099 mptcp_carve_data_frag(const struct mptcp_sock *msk, struct page_frag *pfrag, int orig_offset) argument
1125 mptcp_check_allowed_size(const struct mptcp_sock *msk, struct sock *ssk, u64 data_seq, int avail_size) argument
1210 mptcp_update_infinite_map(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_ext *mpext) argument
1234 struct mptcp_sock *msk = mptcp_sk(sk); local
1407 mptcp_subflow_get_send(struct mptcp_sock *msk) argument
1487 mptcp_update_post_push(struct mptcp_sock *msk, struct mptcp_data_frag *dfrag, u32 sent) argument
1526 struct mptcp_sock *msk = mptcp_sk(sk); local
1570 struct mptcp_sock *msk = mptcp_sk(sk); local
1634 struct mptcp_sock *msk = mptcp_sk(sk); local
1705 struct mptcp_sock *msk = mptcp_sk(sk); local
1776 const struct mptcp_sock *msk = mptcp_sk(sk); local
1795 struct mptcp_sock *msk = mptcp_sk(sk); local
1922 __mptcp_recvmsg_mskq(struct mptcp_sock *msk, struct msghdr *msg, size_t len, int flags, struct scm_timestamping_internal *tss, int *cmsg_flags) argument
1982 mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied) argument
2079 struct mptcp_sock *msk = mptcp_sk(sk); local
2091 struct mptcp_sock *msk = mptcp_sk(sk); local
2096 __mptcp_move_skbs(struct mptcp_sock *msk) argument
2141 const struct mptcp_sock *msk = mptcp_sk(sk); local
2163 struct mptcp_sock *msk = mptcp_sk(sk); local
2280 struct mptcp_sock *msk = mptcp_sk(sk); local
2308 mptcp_subflow_get_retrans(struct mptcp_sock *msk) argument
2347 struct mptcp_sock *msk = mptcp_sk(sk); local
2417 struct mptcp_sock *msk = mptcp_sk(sk); local
2528 struct mptcp_sock *msk = mptcp_sk(sk); local
2557 mptcp_check_fastclose(struct mptcp_sock *msk) argument
2608 struct mptcp_sock *msk = mptcp_sk(sk); local
2688 mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout) argument
2707 mptcp_mp_fail_no_response(struct mptcp_sock *msk) argument
2726 struct mptcp_sock *msk = mptcp_sk(sk); local
2736 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); local
2781 struct mptcp_sock *msk = mptcp_sk(sk); local
2859 struct mptcp_sock *msk = mptcp_sk(sk); local
2869 struct mptcp_sock *msk = mptcp_sk(sk); local
2963 struct mptcp_sock *msk = mptcp_sk(sk); local
2987 struct mptcp_sock *msk = mptcp_sk(sk); local
3002 struct mptcp_sock *msk = mptcp_sk(sk); local
3058 struct mptcp_sock *msk = mptcp_sk(sk); local
3140 mptcp_copy_inaddrs(struct sock *msk, const struct sock *ssk) argument
3165 struct mptcp_sock *msk = mptcp_sk(sk); local
3270 struct mptcp_sock *msk; local
3342 mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk) argument
3359 mptcp_destroy_common(struct mptcp_sock *msk, unsigned int flags) argument
3389 struct mptcp_sock *msk = mptcp_sk(sk); local
3424 struct mptcp_sock *msk = mptcp_sk(sk); variable in typeref:struct:mptcp_sock
3542 struct mptcp_sock *msk = mptcp_sk(sk); local
3554 struct mptcp_sock *msk; local
3586 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
3648 mptcp_ioctl_outq(const struct mptcp_sock *msk, u64 v) argument
3679 struct mptcp_sock *msk = mptcp_sk(sk); local
3709 mptcp_subflow_early_fallback(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow) argument
3719 struct mptcp_sock *msk = mptcp_sk(sk); local
3825 struct mptcp_sock *msk = mptcp_sk(sock->sk); local
3852 struct mptcp_sock *msk = mptcp_sk(sock->sk); local
3893 struct mptcp_sock *msk = mptcp_sk(sock->sk); local
3975 mptcp_check_writeable(struct mptcp_sock *msk) argument
3994 struct mptcp_sock *msk; local
[all...]
H A Dpm_netlink.c52 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) argument
54 return pm_nl_get_pernet(sock_net((struct sock *)msk));
148 const struct mptcp_sock *msk)
152 msk_owned_by_me(msk);
159 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap))
170 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) argument
177 * Note: removal from the local address list during the msk life-cycle
181 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap))
194 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk) argument
196 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk);
147 select_local_address(const struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) argument
202 mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk) argument
210 mptcp_pm_get_subflows_max(const struct mptcp_sock *msk) argument
218 mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk) argument
226 mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk) argument
240 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument
255 mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk) argument
279 struct mptcp_sock *msk = entry->sock; local
321 mptcp_pm_del_add_timer(struct mptcp_sock *msk, const struct mptcp_addr_info *addr, bool check_id) argument
339 mptcp_pm_alloc_anno_list(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument
376 mptcp_pm_free_anno_list(struct mptcp_sock *msk) argument
397 fill_remote_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *local, bool fullmesh, struct mptcp_addr_info *addrs) argument
462 __mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) argument
482 mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) argument
514 mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk) argument
608 mptcp_pm_nl_fully_established(struct mptcp_sock *msk) argument
613 mptcp_pm_nl_subflow_established(struct mptcp_sock *msk) argument
621 fill_local_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *remote, struct mptcp_addr_info *addrs) argument
673 mptcp_pm_nl_add_addr_received(struct mptcp_sock *msk) argument
722 mptcp_pm_nl_addr_send_ack(struct mptcp_sock *msk) argument
738 mptcp_pm_nl_mp_prio_send_ack(struct mptcp_sock *msk, struct mptcp_addr_info *addr, struct mptcp_addr_info *rem, u8 bkup) argument
768 mptcp_local_id_match(const struct mptcp_sock *msk, u8 local_id, u8 id) argument
773 mptcp_pm_nl_rm_addr_or_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list, enum linux_mptcp_mib_field rm_type) argument
843 mptcp_pm_nl_rm_addr_received(struct mptcp_sock *msk) argument
848 mptcp_pm_nl_rm_subflow_received(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument
854 mptcp_pm_nl_work(struct mptcp_sock *msk) argument
1068 mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc) argument
1115 mptcp_pm_nl_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk) argument
1267 struct mptcp_sock *msk; local
1359 mptcp_pm_nl_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument
1377 remove_anno_list_by_saddr(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument
1392 mptcp_pm_remove_anno_addr(struct mptcp_sock *msk, const struct mptcp_addr_info *addr, bool force) argument
1416 struct mptcp_sock *msk; local
1455 struct mptcp_sock *msk; local
1533 mptcp_pm_remove_addrs(struct mptcp_sock *msk, struct list_head *rm_list) argument
1552 mptcp_pm_remove_addrs_and_subflows(struct mptcp_sock *msk, struct list_head *rm_list) argument
1581 struct mptcp_sock *msk; local
1853 mptcp_pm_nl_fullmesh(struct mptcp_sock *msk, struct mptcp_addr_info *addr) argument
1871 struct mptcp_sock *msk; local
1960 mptcp_userspace_pm_active(const struct mptcp_sock *msk) argument
2016 mptcp_event_put_token_and_ssk(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument
2049 mptcp_event_sub_established(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument
2056 mptcp_event_sub_closed(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument
2078 mptcp_event_created(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument
2093 mptcp_event_addr_removed(const struct mptcp_sock *msk, uint8_t id) argument
2128 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
2233 mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk, const struct sock *ssk, gfp_t gfp) argument
[all...]
H A Dfastopen.c62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, argument
65 struct sock *sk = (struct sock *)msk;
71 pr_debug("msk %p moving seq %llx -> %llx end_seq %llx -> %llx", sk,
72 MPTCP_SKB_CB(skb)->map_seq, MPTCP_SKB_CB(skb)->map_seq + msk->ack_seq,
73 MPTCP_SKB_CB(skb)->end_seq, MPTCP_SKB_CB(skb)->end_seq + msk->ack_seq);
74 MPTCP_SKB_CB(skb)->map_seq += msk->ack_seq;
75 MPTCP_SKB_CB(skb)->end_seq += msk->ack_seq;
78 pr_debug("msk=%p ack_seq=%llx", msk, msk
[all...]
H A Dpm_userspace.c11 void mptcp_free_local_addr_list(struct mptcp_sock *msk) argument
14 struct sock *sk = (struct sock *)msk;
17 if (!mptcp_pm_is_userspace(msk))
20 spin_lock_bh(&msk->pm.lock);
21 list_splice_init(&msk->pm.userspace_pm_local_addr_list, &free_list);
22 spin_unlock_bh(&msk->pm.lock);
29 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, argument
35 struct sock *sk = (struct sock *)msk;
43 spin_lock_bh(&msk->pm.lock);
44 list_for_each_entry(e, &msk
90 mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk, struct mptcp_pm_addr_entry *addr) argument
111 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id) argument
122 mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument
139 mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc) argument
173 struct mptcp_sock *msk; local
234 mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk, struct genl_info *info) argument
274 struct mptcp_sock *msk; local
339 struct mptcp_sock *msk; local
413 mptcp_nl_find_ssk(struct mptcp_sock *msk, const struct mptcp_addr_info *local, const struct mptcp_addr_info *remote) argument
468 struct mptcp_sock *msk; local
558 struct mptcp_sock *msk; local
617 struct mptcp_sock *msk; local
675 struct mptcp_sock *msk; local
[all...]
H A Dprotocol.h302 * protected by the msk data lock
353 static inline void msk_owned_by_me(const struct mptcp_sock *msk) argument
355 sock_owned_by_me((const struct sock *)msk);
376 /* the msk socket don't use the backlog, also account for the bulk
396 const struct mptcp_sock *msk = mptcp_sk(sk); local
398 return READ_ONCE(msk->first_pending);
403 struct mptcp_sock *msk = mptcp_sk(sk); local
406 cur = msk->first_pending;
407 return list_is_last(&cur->list, &msk->rtx_queue) ? NULL :
413 const struct mptcp_sock *msk local
426 struct mptcp_sock *msk = mptcp_sk(sk); local
457 struct mptcp_sock *msk; member in struct:mptcp_subflow_request_sock
736 mptcp_data_avail(const struct mptcp_sock *msk) argument
850 mptcp_data_fin_enabled(const struct mptcp_sock *msk) argument
867 const struct mptcp_sock *msk = mptcp_sk(sk); local
1043 mptcp_pm_should_add_signal(struct mptcp_sock *msk) argument
1049 mptcp_pm_should_add_signal_addr(struct mptcp_sock *msk) argument
1054 mptcp_pm_should_add_signal_echo(struct mptcp_sock *msk) argument
1059 mptcp_pm_should_rm_signal(struct mptcp_sock *msk) argument
1064 mptcp_pm_is_userspace(const struct mptcp_sock *msk) argument
1069 mptcp_pm_is_kernel(const struct mptcp_sock *msk) argument
1135 __mptcp_pm_close_subflow(struct mptcp_sock *msk) argument
1141 mptcp_pm_close_subflow(struct mptcp_sock *msk) argument
1158 __mptcp_check_fallback(const struct mptcp_sock *msk) argument
1166 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
1171 __mptcp_do_fallback(struct mptcp_sock *msk) argument
1180 __mptcp_has_initial_subflow(const struct mptcp_sock *msk) argument
1193 struct mptcp_sock *msk; local
[all...]
H A Dtoken.c154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
175 WRITE_ONCE(msk->token, subflow->token);
176 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain);
186 * @msk: the just cloned socket linked to the new connection
192 struct mptcp_sock *msk)
195 struct sock *sk = (struct sock *)msk;
206 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain);
214 struct mptcp_sock *msk; local
222 msk = mptcp_sk(sk);
223 if (READ_ONCE(msk
191 mptcp_token_accept(struct mptcp_subflow_request_sock *req, struct mptcp_sock *msk) argument
250 struct mptcp_sock *msk; local
375 mptcp_token_destroy(struct mptcp_sock *msk) argument
[all...]
H A Dsubflow.c44 if (subflow_req->msk)
45 sock_put((struct sock *)subflow_req->msk);
61 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) argument
63 return mptcp_is_fully_established((void *)msk) &&
64 ((mptcp_pm_is_userspace(msk) &&
65 mptcp_userspace_pm_active(msk)) ||
66 READ_ONCE(msk->pm.accept_subflow));
72 struct mptcp_sock *msk = subflow_req->msk; local
77 subflow_generate_hmac(READ_ONCE(msk
88 struct mptcp_sock *msk; local
119 subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) argument
436 subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) argument
444 struct mptcp_sock *msk = mptcp_sk(sk); local
463 subflow_set_remote_key(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, const struct mptcp_options_received *mp_opt) argument
488 struct mptcp_sock *msk = mptcp_sk(sk); local
514 struct mptcp_sock *msk; local
606 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
729 struct mptcp_sock *msk; local
774 __mptcp_subflow_fully_established(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, const struct mptcp_options_received *mp_opt) argument
1072 get_mapping_status(struct sock *ssk, struct mptcp_sock *msk) argument
1239 subflow_sched_work_if_closed(struct mptcp_sock *msk, struct sock *ssk) argument
1251 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
1261 mptcp_subflow_fail(struct mptcp_sock *msk, struct sock *ssk) argument
1292 struct mptcp_sock *msk; local
1445 struct mptcp_sock *msk; local
1550 struct mptcp_sock *msk = mptcp_sk(sk); local
1790 struct mptcp_sock *msk; local
[all...]
H A Dsyncookies.c86 * Look up the saved state based on skb hash & check token matches msk
89 * Caller will check msk can still accept another subflow. The hmac
97 struct mptcp_sock *msk; local
111 msk = mptcp_token_get_sock(net, e->token);
112 if (!msk) {
122 subflow_req->msk = msk;
H A Dmptcp_diag.c31 struct mptcp_sock *msk = NULL; local
38 msk = mptcp_token_get_sock(net, req->id.idiag_cookie[0]);
39 if (!msk)
43 sk = (struct sock *)msk;
158 struct mptcp_sock *msk; local
166 while ((msk = mptcp_token_iter_next(net, &diag_ctx->s_slot,
168 struct inet_sock *inet = (struct inet_sock *)msk;
169 struct sock *sk = (struct sock *)msk;
202 struct mptcp_sock *msk = mptcp_sk(sk); local
209 struct sock *lsk = READ_ONCE(msk
[all...]
H A Doptions.c449 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
481 opts->csum_reqd = READ_ONCE(msk->csum_enabled);
562 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
569 opts->csum_reqd = READ_ONCE(msk->csum_enabled);
589 /* passive sockets msk will set the 'can_ack' after accept(), even
593 if (!READ_ONCE(msk->can_ack)) {
598 ack_seq = READ_ONCE(msk->ack_seq);
599 if (READ_ONCE(msk->use_64bit_ack)) {
610 WRITE_ONCE(msk->old_wspace, __mptcp_space((struct sock *)msk));
655 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
710 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
785 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
830 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
925 check_fully_established(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_subflow_context *subflow, struct sk_buff *skb, struct mptcp_options_received *mp_opt) argument
1031 __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) argument
1037 ack_update_msk(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_options_received *mp_opt) argument
1079 mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) argument
1096 add_addr_hmac_valid(struct mptcp_sock *msk, struct mptcp_options_received *mp_opt) argument
1118 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local
1256 struct mptcp_sock *msk; local
[all...]
/linux-master/drivers/net/ethernet/netronome/nfp/flower/
H A Dmatch.c12 struct nfp_flower_meta_tci *msk, u8 key_type)
18 msk->nfp_flow_key_layer = key_type;
19 msk->mask_id = ~0;
24 struct nfp_flower_meta_tci *msk,
47 msk->tci |= cpu_to_be16(msk_tci);
53 struct nfp_flower_meta_tci *msk,
57 memset(msk, 0, sizeof(struct nfp_flower_meta_tci));
59 nfp_flower_compile_meta(ext, msk, key_type);
62 nfp_flower_compile_tci(ext, msk, rule);
96 struct nfp_flower_mac_mpls *msk,
11 nfp_flower_compile_meta(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, u8 key_type) argument
23 nfp_flower_compile_tci(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, struct flow_rule *rule) argument
52 nfp_flower_compile_meta_tci(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, struct flow_rule *rule, u8 key_type, bool qinq_sup) argument
95 nfp_flower_compile_mac(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule) argument
119 nfp_flower_compile_mpls(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, struct netlink_ext_ack *extack) argument
174 nfp_flower_compile_mac_mpls(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, struct netlink_ext_ack *extack) argument
188 nfp_flower_compile_tport(struct nfp_flower_tp_ports *ext, struct nfp_flower_tp_ports *msk, struct flow_rule *rule) argument
209 nfp_flower_compile_ip_ext(struct nfp_flower_ip_ext *ext, struct nfp_flower_ip_ext *msk, struct flow_rule *rule) argument
285 nfp_flower_fill_vlan(struct flow_match_vlan *match, struct nfp_flower_vlan *ext, struct nfp_flower_vlan *msk, bool outer_vlan) argument
318 nfp_flower_compile_vlan(struct nfp_flower_vlan *ext, struct nfp_flower_vlan *msk, struct flow_rule *rule) argument
335 nfp_flower_compile_ipv4(struct nfp_flower_ipv4 *ext, struct nfp_flower_ipv4 *msk, struct flow_rule *rule) argument
357 nfp_flower_compile_ipv6(struct nfp_flower_ipv6 *ext, struct nfp_flower_ipv6 *msk, struct flow_rule *rule) argument
385 nfp_flower_compile_geneve_opt(u8 *ext, u8 *msk, struct flow_rule *rule) argument
401 nfp_flower_compile_tun_ipv4_addrs(struct nfp_flower_tun_ipv4 *ext, struct nfp_flower_tun_ipv4 *msk, struct flow_rule *rule) argument
417 nfp_flower_compile_tun_ipv6_addrs(struct nfp_flower_tun_ipv6 *ext, struct nfp_flower_tun_ipv6 *msk, struct flow_rule *rule) argument
438 nfp_flower_compile_tun_ip_ext(struct nfp_flower_tun_ip_ext *ext, struct nfp_flower_tun_ip_ext *msk, struct flow_rule *rule) argument
487 nfp_flower_compile_ipv4_gre_tun(struct nfp_flower_ipv4_gre_tun *ext, struct nfp_flower_ipv4_gre_tun *msk, struct flow_rule *rule) argument
502 nfp_flower_compile_ipv4_udp_tun(struct nfp_flower_ipv4_udp_tun *ext, struct nfp_flower_ipv4_udp_tun *msk, struct flow_rule *rule) argument
512 nfp_flower_compile_ipv6_udp_tun(struct nfp_flower_ipv6_udp_tun *ext, struct nfp_flower_ipv6_udp_tun *msk, struct flow_rule *rule) argument
522 nfp_flower_compile_ipv6_gre_tun(struct nfp_flower_ipv6_gre_tun *ext, struct nfp_flower_ipv6_gre_tun *msk, struct flow_rule *rule) argument
550 u8 *msk; local
[all...]
/linux-master/tools/testing/selftests/bpf/progs/
H A Dmptcp_sock.c32 struct mptcp_sock *msk; local
60 msk = bpf_skc_to_mptcp_sock(sk);
61 if (!msk)
64 storage = bpf_sk_storage_get(&socket_storage_map, msk, 0,
69 storage->token = msk->token;
70 __builtin_memcpy(storage->ca_name, msk->ca_name, TCP_CA_NAME_MAX);
71 storage->first = msk->first;
81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk, argument
85 token = msk->token;
/linux-master/drivers/media/usb/pvrusb2/
H A Dpvrusb2-debug.h11 #define pvr2_trace(msk, fmt, arg...) do {if (msk & pvrusb2_debug) pr_info("pvrusb2: " fmt "\n", ##arg); } while (0)
/linux-master/net/mctp/
H A Daf_mctp.c55 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local
81 msk->bind_net = smctp->smctp_network;
82 msk->bind_addr = smctp->smctp_addr.s_addr;
83 msk->bind_type = smctp->smctp_type & 0x7f; /* ignore the IC bit */
98 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local
133 if (msk->addr_ext && addrlen >= sizeof(struct sockaddr_mctp_ext)) {
210 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local
259 if (msk->addr_ext) {
311 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local
322 msk
332 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local
424 mctp_ioctl_alloctag(struct mctp_sock *msk, bool tagv2, unsigned long arg) argument
467 mctp_ioctl_droptag(struct mctp_sock *msk, bool tagv2, unsigned long arg) argument
513 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local
572 struct mctp_sock *msk = container_of(timer, struct mctp_sock, local
614 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local
639 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local
[all...]
/linux-master/drivers/net/ethernet/aquantia/atlantic/
H A Daq_hw_utils.c19 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, argument
22 if (msk ^ ~0) {
26 reg_new = (reg_old & (~msk)) | (val << shift);
35 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) argument
37 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift);
/linux-master/kernel/irq/
H A Ddevres.c235 u32 msk; member in struct:irq_generic_chip_devres
244 irq_remove_generic_chip(this->gc, this->msk, this->clr, this->set);
253 * @msk: Bitmask holding the irqs to initialize relative to gc->irq_base
263 u32 msk, enum irq_gc_flags flags,
273 irq_setup_generic_chip(gc, msk, flags, clr, set);
276 dr->msk = msk;
262 devm_irq_setup_generic_chip(struct device *dev, struct irq_chip_generic *gc, u32 msk, enum irq_gc_flags flags, unsigned int clr, unsigned int set) argument
H A Dmatrix.c136 const struct cpumask *msk)
143 for_each_cpu(cpu, msk) {
157 const struct cpumask *msk)
164 for_each_cpu(cpu, msk) {
210 * @msk: On which CPUs the bits should be reserved.
213 * on all CPUs in @msk, but it's not guaranteed that the bits are at the
216 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) argument
220 for_each_cpu(cpu, msk) {
237 for_each_cpu(cpu, msk) {
248 * @msk
135 matrix_find_best_cpu(struct irq_matrix *m, const struct cpumask *msk) argument
156 matrix_find_best_cpu_managed(struct irq_matrix *m, const struct cpumask *msk) argument
257 irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) argument
292 irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, unsigned int *mapped_cpu) argument
383 irq_matrix_alloc(struct irq_matrix *m, const struct cpumask *msk, bool reserved, unsigned int *mapped_cpu) argument
[all...]
/linux-master/drivers/clk/sprd/
H A Dpll.c54 u32 msk, u32 val)
66 regmap_write(common->regmap, offset, (reg & ~msk) | val);
173 cfg[index].msk = mask;
184 cfg[index].msk |= mask;
189 cfg[index].msk |= mask;
196 cfg[index].msk |= mask;
206 cfg[index].msk |= mask;
214 cfg[index].msk |= mask;
217 if (cfg[i].msk) {
218 sprd_pll_write(pll, i, cfg[i].msk, cf
53 sprd_pll_write(const struct sprd_pll *pll, u8 index, u32 msk, u32 val) argument
[all...]
/linux-master/drivers/usb/mtu3/
H A Dmtu3_host.c70 u32 reg, msk, val; local
75 msk = WC1_IS_EN | WC1_IS_C(0xf) | WC1_IS_P;
80 msk = WC0_IS_EN | WC0_IS_C(0xf) | WC0_IS_P;
85 msk = WC0_SSUSB0_CDEN | WC0_IS_SPM_EN;
86 val = enable ? msk : 0;
90 msk = WC1_IS_EN_P0_95 | WC1_IS_C_95(0xf) | WC1_IS_P_95;
95 msk = WC0_IS_EN_P2_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95;
100 msk = WC0_IS_EN_P3_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95;
105 msk = SSC_IP_SLEEP_EN | SSC_SPM_INT_EN;
106 val = enable ? msk
[all...]

Completed in 465 milliseconds

123456