Symbol: mptcp_sock
include/linux/btf_ids.h
257
BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
include/net/mptcp.h
105
int (*get_send)(struct mptcp_sock *msk);
include/net/mptcp.h
106
int (*get_retrans)(struct mptcp_sock *msk);
include/net/mptcp.h
112
void (*init)(struct mptcp_sock *msk);
include/net/mptcp.h
113
void (*release)(struct mptcp_sock *msk);
include/net/mptcp.h
125
void (*init)(struct mptcp_sock *msk);
include/net/mptcp.h
126
void (*release)(struct mptcp_sock *msk);
include/net/mptcp.h
16
struct mptcp_sock;
include/net/mptcp.h
160
void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
include/net/mptcp.h
331
struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
include/net/mptcp.h
333
static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; }
include/trace/events/mptcp.h
216
struct mptcp_sock *msk = mptcp_sk(sk);
net/core/filter.c
12050
BTF_TYPE_EMIT(struct mptcp_sock);
net/mptcp/bpf.c
15
struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk)
net/mptcp/mptcp_diag.c
155
struct mptcp_sock *msk;
net/mptcp/mptcp_diag.c
195
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/mptcp_diag.c
31
struct mptcp_sock *msk = NULL;
net/mptcp/options.c
1051
static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una)
net/mptcp/options.c
1057
static void rwin_update(struct mptcp_sock *msk, struct sock *ssk,
net/mptcp/options.c
1082
static void ack_update_msk(struct mptcp_sock *msk,
net/mptcp/options.c
1124
bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit)
net/mptcp/options.c
1141
static bool add_addr_hmac_valid(struct mptcp_sock *msk,
net/mptcp/options.c
1165
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
1304
struct mptcp_sock *msk;
net/mptcp/options.c
1370
struct mptcp_sock *msk;
net/mptcp/options.c
455
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
568
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
660
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
724
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
799
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
844
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
942
static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk,
net/mptcp/pm.c
1008
void mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/pm.c
1027
void mptcp_pm_worker(struct mptcp_sock *msk)
net/mptcp/pm.c
1052
void mptcp_pm_destroy(struct mptcp_sock *msk)
net/mptcp/pm.c
1060
void mptcp_pm_data_reset(struct mptcp_sock *msk)
net/mptcp/pm.c
108
static bool mptcp_pm_is_init_remote_addr(struct mptcp_sock *msk,
net/mptcp/pm.c
1089
void mptcp_pm_data_init(struct mptcp_sock *msk)
net/mptcp/pm.c
136
mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk,
net/mptcp/pm.c
151
bool mptcp_remove_anno_list_by_saddr(struct mptcp_sock *msk,
net/mptcp/pm.c
164
bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk)
net/mptcp/pm.c
185
static void __mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
20
struct mptcp_sock *sock;
net/mptcp/pm.c
206
void mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
229
mptcp_pm_addr_send_ack_avoid_list(struct mptcp_sock *msk,
net/mptcp/pm.c
268
void mptcp_pm_addr_send_ack(struct mptcp_sock *msk)
net/mptcp/pm.c
273
int mptcp_pm_mp_prio_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
303
static unsigned int mptcp_adjust_add_addr_timeout(struct mptcp_sock *msk)
net/mptcp/pm.c
328
struct mptcp_sock *msk = entry->sock;
net/mptcp/pm.c
375
mptcp_pm_del_add_timer(struct mptcp_sock *msk,
net/mptcp/pm.c
404
bool mptcp_pm_alloc_anno_list(struct mptcp_sock *msk,
net/mptcp/pm.c
441
static void mptcp_pm_free_anno_list(struct mptcp_sock *msk)
net/mptcp/pm.c
461
int mptcp_pm_announce_addr(struct mptcp_sock *msk,
net/mptcp/pm.c
489
int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list)
net/mptcp/pm.c
510
void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side)
net/mptcp/pm.c
520
bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk)
net/mptcp/pm.c
560
static bool mptcp_pm_schedule_work(struct mptcp_sock *msk,
net/mptcp/pm.c
573
void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk)
net/mptcp/pm.c
600
void mptcp_pm_connection_closed(struct mptcp_sock *msk)
net/mptcp/pm.c
608
void mptcp_pm_subflow_established(struct mptcp_sock *msk)
net/mptcp/pm.c
625
void mptcp_pm_subflow_check_next(struct mptcp_sock *msk,
net/mptcp/pm.c
663
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/pm.c
697
void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk,
net/mptcp/pm.c
715
void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk)
net/mptcp/pm.c
723
static void mptcp_pm_rm_addr_or_subflow(struct mptcp_sock *msk,
net/mptcp/pm.c
786
static void mptcp_pm_rm_addr_recv(struct mptcp_sock *msk)
net/mptcp/pm.c
791
void mptcp_pm_rm_subflow(struct mptcp_sock *msk,
net/mptcp/pm.c
797
void mptcp_pm_rm_addr_received(struct mptcp_sock *msk,
net/mptcp/pm.c
820
struct mptcp_sock *msk;
net/mptcp/pm.c
833
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/pm.c
858
bool mptcp_pm_add_addr_signal(struct mptcp_sock *msk, const struct sk_buff *skb,
net/mptcp/pm.c
905
bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
net/mptcp/pm.c
935
int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc)
net/mptcp/pm.c
959
bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc)
net/mptcp/pm.c
971
static void mptcp_pm_subflows_chk_stale(const struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/pm_kernel.c
1056
static void mptcp_pm_remove_anno_addr(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1075
static void __mark_subflow_endp_available(struct mptcp_sock *msk, u8 id)
net/mptcp/pm_kernel.c
1089
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
1133
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
121
const struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1225
static void mptcp_pm_flush_addrs_and_subflows(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1258
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
1450
static void mptcp_pm_nl_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1471
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
149
select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1555
bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
1569
void __mptcp_pm_kernel_worker(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
180
fill_remote_addr(struct mptcp_sock *msk, struct mptcp_addr_info *local,
net/mptcp/pm_kernel.c
202
fill_remote_addresses_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
250
fill_remote_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *local,
net/mptcp/pm_kernel.c
289
static u8 mptcp_endp_get_local_id(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
296
static void mptcp_mpc_endpoint_setup(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
329
static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
40
pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
433
static void mptcp_pm_nl_fully_established(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
438
static void mptcp_pm_nl_subflow_established(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
444
fill_local_addresses_vec_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
497
fill_local_laminar_endp(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
50
u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
557
fill_local_addresses_vec_c_flag(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
58
u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
594
fill_local_address_any(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
619
fill_local_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
643
static void mptcp_pm_nl_add_addr_received(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
66
u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
692
void mptcp_pm_nl_rm_addr(struct mptcp_sock *msk, u8 rm_id)
net/mptcp/pm_kernel.c
74
u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
82
u8 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
90
u8 mptcp_pm_get_limit_extra_subflows(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
904
int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
933
bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc)
net/mptcp/pm_kernel.c
950
struct mptcp_sock *msk;
net/mptcp/pm_netlink.c
291
bool mptcp_userspace_pm_active(const struct mptcp_sock *msk)
net/mptcp/pm_netlink.c
346
const struct mptcp_sock *msk,
net/mptcp/pm_netlink.c
379
const struct mptcp_sock *msk,
net/mptcp/pm_netlink.c
386
const struct mptcp_sock *msk,
net/mptcp/pm_netlink.c
408
const struct mptcp_sock *msk,
net/mptcp/pm_netlink.c
434
void mptcp_event_addr_removed(const struct mptcp_sock *msk, uint8_t id)
net/mptcp/pm_netlink.c
469
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/pm_netlink.c
572
void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
118
mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id)
net/mptcp/pm_userspace.c
129
int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
148
bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
15
void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk)
net/mptcp/pm_userspace.c
162
static struct mptcp_sock *mptcp_userspace_pm_get_sock(const struct genl_info *info)
net/mptcp/pm_userspace.c
164
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
190
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
246
static int mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk)
net/mptcp/pm_userspace.c
277
void mptcp_pm_remove_addr_entry(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
300
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
31
mptcp_userspace_pm_lookup_addr(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
363
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
43
static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
430
static struct sock *mptcp_nl_find_ssk(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
481
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
561
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
629
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
666
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
98
static int mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk,
net/mptcp/protocol.c
1004
static bool mptcp_frag_can_collapse_to(const struct mptcp_sock *msk,
net/mptcp/protocol.c
103
static int __mptcp_socket_create(struct mptcp_sock *msk)
net/mptcp/protocol.c
1032
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1107
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1137
mptcp_carve_data_frag(const struct mptcp_sock *msk, struct page_frag *pfrag,
net/mptcp/protocol.c
1163
static size_t mptcp_check_allowed_size(const struct mptcp_sock *msk,
net/mptcp/protocol.c
1249
static void mptcp_update_infinite_map(struct mptcp_sock *msk,
net/mptcp/protocol.c
1276
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
133
struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk)
net/mptcp/protocol.c
1455
struct sock *mptcp_subflow_get_send(struct mptcp_sock *msk)
net/mptcp/protocol.c
1537
static void mptcp_update_post_push(struct mptcp_sock *msk,
net/mptcp/protocol.c
1576
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1620
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1687
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1758
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1831
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1848
static void mptcp_rps_record_subflows(const struct mptcp_sock *msk)
net/mptcp/protocol.c
1864
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
195
static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to,
net/mptcp/protocol.c
1993
static void mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied);
net/mptcp/protocol.c
2011
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2074
static void mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk)
net/mptcp/protocol.c
2093
static void mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied)
net/mptcp/protocol.c
210
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2170
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2198
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2219
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2245
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2267
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2382
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2412
struct sock *mptcp_subflow_get_retrans(struct mptcp_sock *msk)
net/mptcp/protocol.c
243
static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb)
net/mptcp/protocol.c
2451
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2520
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2622
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2661
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2694
static void mptcp_check_fastclose(struct mptcp_sock *msk)
net/mptcp/protocol.c
2746
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2851
void mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout)
net/mptcp/protocol.c
2870
static void mptcp_mp_fail_no_response(struct mptcp_sock *msk)
net/mptcp/protocol.c
2888
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2907
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2942
struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work);
net/mptcp/protocol.c
2991
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3073
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3083
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3177
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3201
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3216
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3270
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3374
static void mptcp_destroy_common(struct mptcp_sock *msk)
net/mptcp/protocol.c
3398
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3513
struct mptcp_sock *msk;
net/mptcp/protocol.c
3588
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3620
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3746
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3758
struct mptcp_sock *msk;
net/mptcp/protocol.c
379
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
38
struct mptcp_sock msk;
net/mptcp/protocol.c
3807
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/protocol.c
3879
static int mptcp_ioctl_outq(const struct mptcp_sock *msk, u64 v)
net/mptcp/protocol.c
3910
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3945
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4047
.obj_size = sizeof(struct mptcp_sock),
net/mptcp/protocol.c
4054
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4081
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4122
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4185
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4260
static __poll_t mptcp_check_writeable(struct mptcp_sock *msk)
net/mptcp/protocol.c
427
static void mptcp_shutdown_subflows(struct mptcp_sock *msk)
net/mptcp/protocol.c
4279
struct mptcp_sock *msk;
net/mptcp/protocol.c
4326
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4351
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
444
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
453
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
477
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
550
static void mptcp_send_ack(struct mptcp_sock *msk)
net/mptcp/protocol.c
581
static void mptcp_cleanup_rbuf(struct mptcp_sock *msk, int copied)
net/mptcp/protocol.c
59
static u64 mptcp_wnd_end(const struct mptcp_sock *msk)
net/mptcp/protocol.c
602
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
648
static void mptcp_dss_corruption(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
660
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
698
static bool __mptcp_move_skbs_from_subflow(struct mptcp_sock *msk,
net/mptcp/protocol.c
76
bool __mptcp_try_fallback(struct mptcp_sock *msk, int fb_mib)
net/mptcp/protocol.c
773
static bool __mptcp_ofo_queue(struct mptcp_sock *msk)
net/mptcp/protocol.c
852
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
862
static bool move_skbs_to_msk(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
885
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
905
static void mptcp_subflow_joined(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
912
static bool __mptcp_finish_join(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
937
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
1042
struct mptcp_sock *msk);
net/mptcp/protocol.h
1044
struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token);
net/mptcp/protocol.h
1045
struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot,
net/mptcp/protocol.h
1047
void mptcp_token_destroy(struct mptcp_sock *msk);
net/mptcp/protocol.h
1055
void mptcp_pm_data_init(struct mptcp_sock *msk);
net/mptcp/protocol.h
1056
void mptcp_pm_data_reset(struct mptcp_sock *msk);
net/mptcp/protocol.h
1057
void mptcp_pm_destroy(struct mptcp_sock *msk);
net/mptcp/protocol.h
1066
void mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk);
net/mptcp/protocol.h
1067
void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side);
net/mptcp/protocol.h
1068
void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk);
net/mptcp/protocol.h
1069
bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk);
net/mptcp/protocol.h
1070
void mptcp_pm_connection_closed(struct mptcp_sock *msk);
net/mptcp/protocol.h
1071
void mptcp_pm_subflow_established(struct mptcp_sock *msk);
net/mptcp/protocol.h
1072
bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk);
net/mptcp/protocol.h
1073
void mptcp_pm_subflow_check_next(struct mptcp_sock *msk,
net/mptcp/protocol.h
1077
void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk,
net/mptcp/protocol.h
1079
void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk);
net/mptcp/protocol.h
1080
void mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/protocol.h
1083
void mptcp_pm_addr_send_ack(struct mptcp_sock *msk);
net/mptcp/protocol.h
1084
void mptcp_pm_nl_rm_addr(struct mptcp_sock *msk, u8 rm_id);
net/mptcp/protocol.h
1085
void mptcp_pm_rm_subflow(struct mptcp_sock *msk,
net/mptcp/protocol.h
1087
void mptcp_pm_rm_addr_received(struct mptcp_sock *msk,
net/mptcp/protocol.h
1091
int mptcp_pm_mp_prio_send_ack(struct mptcp_sock *msk,
net/mptcp/protocol.h
1095
bool mptcp_pm_alloc_anno_list(struct mptcp_sock *msk,
net/mptcp/protocol.h
1097
bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk);
net/mptcp/protocol.h
1099
mptcp_pm_del_add_timer(struct mptcp_sock *msk,
net/mptcp/protocol.h
1103
bool mptcp_remove_anno_list_by_saddr(struct mptcp_sock *msk,
net/mptcp/protocol.h
1109
int mptcp_pm_announce_addr(struct mptcp_sock *msk,
net/mptcp/protocol.h
1112
int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list);
net/mptcp/protocol.h
1113
void mptcp_pm_remove_addr_entry(struct mptcp_sock *msk,
net/mptcp/protocol.h
1125
void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk);
net/mptcp/protocol.h
1127
void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk,
net/mptcp/protocol.h
1130
void mptcp_event_addr_removed(const struct mptcp_sock *msk, u8 id);
net/mptcp/protocol.h
1133
bool mptcp_userspace_pm_active(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1141
static inline bool mptcp_pm_should_add_signal(struct mptcp_sock *msk)
net/mptcp/protocol.h
1147
static inline bool mptcp_pm_should_add_signal_addr(struct mptcp_sock *msk)
net/mptcp/protocol.h
1152
static inline bool mptcp_pm_should_add_signal_echo(struct mptcp_sock *msk)
net/mptcp/protocol.h
1157
static inline bool mptcp_pm_should_rm_signal(struct mptcp_sock *msk)
net/mptcp/protocol.h
1162
static inline bool mptcp_pm_is_userspace(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1167
static inline bool mptcp_pm_is_kernel(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1195
bool mptcp_pm_add_addr_signal(struct mptcp_sock *msk, const struct sk_buff *skb,
net/mptcp/protocol.h
1199
bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
net/mptcp/protocol.h
1201
int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
net/mptcp/protocol.h
1202
int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk,
net/mptcp/protocol.h
1204
int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk,
net/mptcp/protocol.h
1206
bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
net/mptcp/protocol.h
1207
bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
net/mptcp/protocol.h
1208
bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
net/mptcp/protocol.h
1230
void mptcp_pm_worker(struct mptcp_sock *msk);
net/mptcp/protocol.h
1231
void __mptcp_pm_kernel_worker(struct mptcp_sock *msk);
net/mptcp/protocol.h
1232
u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1233
u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1234
u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1235
u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1236
u8 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1237
u8 mptcp_pm_get_limit_extra_subflows(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1240
static inline void __mptcp_pm_close_subflow(struct mptcp_sock *msk)
net/mptcp/protocol.h
1246
static inline void mptcp_pm_close_subflow(struct mptcp_sock *msk)
net/mptcp/protocol.h
1253
static inline bool mptcp_pm_add_addr_c_flag_case(struct mptcp_sock *msk)
net/mptcp/protocol.h
1261
void mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk);
net/mptcp/protocol.h
1270
static inline bool __mptcp_check_fallback(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1278
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/protocol.h
1283
static inline bool __mptcp_has_initial_subflow(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1292
bool __mptcp_try_fallback(struct mptcp_sock *msk, int fb_mib);
net/mptcp/protocol.h
1298
struct mptcp_sock *msk;
net/mptcp/protocol.h
1317
static inline void mptcp_early_fallback(struct mptcp_sock *msk,
net/mptcp/protocol.h
378
static inline void msk_owned_by_me(const struct mptcp_sock *msk)
net/mptcp/protocol.h
394
container_of_const(_ptr, struct mptcp_sock, sk.icsk_inet.sk); \
net/mptcp/protocol.h
398
#define mptcp_sk(ptr) container_of_const(ptr, struct mptcp_sock, sk.icsk_inet.sk)
net/mptcp/protocol.h
420
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
427
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
437
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
450
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
482
struct mptcp_sock *msk;
net/mptcp/protocol.h
771
void __mptcp_subflow_fully_established(struct mptcp_sock *msk,
net/mptcp/protocol.h
786
struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk);
net/mptcp/protocol.h
812
int mptcp_init_sched(struct mptcp_sock *msk,
net/mptcp/protocol.h
814
void mptcp_release_sched(struct mptcp_sock *msk);
net/mptcp/protocol.h
817
struct sock *mptcp_subflow_get_send(struct mptcp_sock *msk);
net/mptcp/protocol.h
818
struct sock *mptcp_subflow_get_retrans(struct mptcp_sock *msk);
net/mptcp/protocol.h
819
int mptcp_sched_get_send(struct mptcp_sock *msk);
net/mptcp/protocol.h
820
int mptcp_sched_get_retrans(struct mptcp_sock *msk);
net/mptcp/protocol.h
822
static inline u64 mptcp_data_avail(const struct mptcp_sock *msk)
net/mptcp/protocol.h
889
void mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout);
net/mptcp/protocol.h
942
bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit);
net/mptcp/protocol.h
943
static inline bool mptcp_data_fin_enabled(const struct mptcp_sock *msk)
net/mptcp/protocol.h
960
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/sched.c
130
int mptcp_init_sched(struct mptcp_sock *msk,
net/mptcp/sched.c
148
void mptcp_release_sched(struct mptcp_sock *msk)
net/mptcp/sched.c
168
int mptcp_sched_get_send(struct mptcp_sock *msk)
net/mptcp/sched.c
19
static int mptcp_sched_default_get_send(struct mptcp_sock *msk)
net/mptcp/sched.c
195
int mptcp_sched_get_retrans(struct mptcp_sock *msk)
net/mptcp/sched.c
31
static int mptcp_sched_default_get_retrans(struct mptcp_sock *msk)
net/mptcp/sockopt.c
1019
static int mptcp_getsockopt_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen)
net/mptcp/sockopt.c
1103
static int mptcp_getsockopt_tcpinfo(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
1195
static int mptcp_getsockopt_subflow_addrs(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
123
static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
1293
static int mptcp_getsockopt_full_info(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
1367
static int mptcp_put_int_option(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
138
static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
1396
static int mptcp_getsockopt_sol_tcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1442
static int mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1467
static int mptcp_getsockopt_v6(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
147
static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
1487
static int mptcp_getsockopt_sol_mptcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1507
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/sockopt.c
1535
static void sync_socket_options(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/sockopt.c
1591
void mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/sockopt.c
172
static int mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
20
static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk)
net/mptcp/sockopt.c
205
static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk,
net/mptcp/sockopt.c
249
static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval,
net/mptcp/sockopt.c
290
static int mptcp_setsockopt_sol_socket(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
387
static int mptcp_setsockopt_v6(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
51
static void sockopt_seq_inc(struct mptcp_sock *msk)
net/mptcp/sockopt.c
58
static int mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval,
net/mptcp/sockopt.c
582
static int mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock *msk, sockptr_t optval,
net/mptcp/sockopt.c
625
static int __mptcp_setsockopt_set_val(struct mptcp_sock *msk, int max,
net/mptcp/sockopt.c
650
static int __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
670
static int __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
689
static int mptcp_setsockopt_sol_ip_set(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
70
static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
735
static int mptcp_setsockopt_v4_set_tos(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
763
static int mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
779
static int mptcp_setsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname,
net/mptcp/sockopt.c
801
static int mptcp_setsockopt_all_sf(struct mptcp_sock *msk, int level,
net/mptcp/sockopt.c
818
static int mptcp_setsockopt_sol_tcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
895
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/sockopt.c
930
static int mptcp_getsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname,
net/mptcp/sockopt.c
956
void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info)
net/mptcp/subflow.c
1110
struct mptcp_sock *msk)
net/mptcp/subflow.c
120
static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk)
net/mptcp/subflow.c
1289
static void subflow_sched_work_if_closed(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/subflow.c
1315
static bool mptcp_subflow_fail(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/subflow.c
1356
struct mptcp_sock *msk;
net/mptcp/subflow.c
1511
struct mptcp_sock *msk;
net/mptcp/subflow.c
1616
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/subflow.c
452
static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk)
net/mptcp/subflow.c
460
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/subflow.c
477
static void subflow_set_remote_key(struct mptcp_sock *msk,
net/mptcp/subflow.c
505
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/subflow.c
531
struct mptcp_sock *msk;
net/mptcp/subflow.c
61
static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk)
net/mptcp/subflow.c
633
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/subflow.c
72
struct mptcp_sock *msk = subflow_req->msk;
net/mptcp/subflow.c
756
struct mptcp_sock *msk = subflow_req->msk;
net/mptcp/subflow.c
797
void __mptcp_subflow_fully_established(struct mptcp_sock *msk,
net/mptcp/subflow.c
820
struct mptcp_sock *owner;
net/mptcp/subflow.c
85
static struct mptcp_sock *subflow_token_join_request(struct request_sock *req)
net/mptcp/subflow.c
88
struct mptcp_sock *msk;
net/mptcp/syncookies.c
97
struct mptcp_sock *msk;
net/mptcp/token.c
154
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/token.c
192
struct mptcp_sock *msk)
net/mptcp/token.c
214
struct mptcp_sock *msk;
net/mptcp/token.c
246
struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token)
net/mptcp/token.c
250
struct mptcp_sock *msk;
net/mptcp/token.c
299
struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot,
net/mptcp/token.c
302
struct mptcp_sock *ret = NULL;
net/mptcp/token.c
377
void mptcp_token_destroy(struct mptcp_sock *msk)
net/mptcp/token.c
381
struct mptcp_sock *pos;
net/mptcp/token.c
67
static struct mptcp_sock *
net/mptcp/token_test.c
116
struct mptcp_sock *msk = build_msk(test);
net/mptcp/token_test.c
117
struct mptcp_sock *null_msk = NULL;
net/mptcp/token_test.c
21
struct mptcp_sock *null_msk = NULL;
net/mptcp/token_test.c
52
static struct mptcp_sock *build_msk(struct kunit *test)
net/mptcp/token_test.c
54
struct mptcp_sock *msk;
net/mptcp/token_test.c
57
msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER);
net/mptcp/token_test.c
75
struct mptcp_sock *msk = build_msk(test);
net/mptcp/token_test.c
76
struct mptcp_sock *null_msk = NULL;
net/mptcp/token_test.c
97
struct mptcp_sock *msk = build_msk(test);
tools/include/linux/btf_ids.h
192
BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
tools/testing/selftests/bpf/prog_tests/mptcp.c
159
struct mptcp_sock *sock_skel;
tools/testing/selftests/bpf/progs/mptcp_sock.c
32
struct mptcp_sock *msk;
tools/testing/selftests/bpf/progs/mptcp_sock.c
81
int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk,
tools/testing/selftests/bpf/progs/mptcp_subflow.c
109
struct mptcp_sock *msk;
tools/testing/selftests/bpf/progs/mptcp_subflow.c
119
msk = bpf_core_cast(sk, struct mptcp_sock);
tools/testing/selftests/bpf/progs/mptcp_subflow.c
26
struct mptcp_sock *msk;
tools/testing/selftests/bpf/progs/mptcp_subflow.c
63
static int _check_getsockopt_subflow_mark(struct mptcp_sock *msk, struct bpf_sockopt *ctx)
tools/testing/selftests/bpf/progs/mptcp_subflow.c
83
static int _check_getsockopt_subflow_cc(struct mptcp_sock *msk, struct bpf_sockopt *ctx)