include/linux/btf_ids.h
257
BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
include/net/mptcp.h
109
int (*get_send)(struct mptcp_sock *msk);
include/net/mptcp.h
110
int (*get_retrans)(struct mptcp_sock *msk);
include/net/mptcp.h
116
void (*init)(struct mptcp_sock *msk);
include/net/mptcp.h
117
void (*release)(struct mptcp_sock *msk);
include/net/mptcp.h
129
void (*init)(struct mptcp_sock *msk);
include/net/mptcp.h
130
void (*release)(struct mptcp_sock *msk);
include/net/mptcp.h
16
struct mptcp_sock;
include/net/mptcp.h
164
void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
include/net/mptcp.h
326
struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
include/net/mptcp.h
328
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
12171
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
1021
static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una)
net/mptcp/options.c
1027
static void rwin_update(struct mptcp_sock *msk, struct sock *ssk,
net/mptcp/options.c
1053
static void ack_update_msk(struct mptcp_sock *msk,
net/mptcp/options.c
1095
bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit)
net/mptcp/options.c
1112
static bool add_addr_hmac_valid(struct mptcp_sock *msk,
net/mptcp/options.c
1136
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
1269
static u64 mptcp_set_rwin(struct mptcp_sock *msk, struct tcp_sock *tp,
net/mptcp/options.c
1336
struct mptcp_sock *msk;
net/mptcp/options.c
1441
struct mptcp_sock *msk;
net/mptcp/options.c
454
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
566
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
663
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
702
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
768
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
812
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/options.c
912
static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk,
net/mptcp/pm.c
1027
int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc)
net/mptcp/pm.c
1051
bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc)
net/mptcp/pm.c
1063
static void mptcp_pm_subflows_chk_stale(const struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/pm.c
109
static bool mptcp_pm_is_init_remote_addr(struct mptcp_sock *msk,
net/mptcp/pm.c
1100
void mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/pm.c
1119
void mptcp_pm_worker(struct mptcp_sock *msk)
net/mptcp/pm.c
1144
void mptcp_pm_destroy(struct mptcp_sock *msk)
net/mptcp/pm.c
1152
void mptcp_pm_data_reset(struct mptcp_sock *msk)
net/mptcp/pm.c
118
bool mptcp_pm_has_subflow_saddr(const struct mptcp_sock *msk,
net/mptcp/pm.c
1181
void mptcp_pm_data_init(struct mptcp_sock *msk)
net/mptcp/pm.c
137
mptcp_pm_announced_lookup(const struct mptcp_sock *msk,
net/mptcp/pm.c
153
mptcp_pm_announced_del_timer(struct mptcp_sock *msk,
net/mptcp/pm.c
186
bool mptcp_pm_announced_remove(struct mptcp_sock *msk,
net/mptcp/pm.c
199
bool mptcp_pm_announced_has_ssk(struct mptcp_sock *msk, const struct sock *ssk)
net/mptcp/pm.c
21
struct mptcp_sock *sock;
net/mptcp/pm.c
220
static void __mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
241
void mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
263
static void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk);
net/mptcp/pm.c
265
mptcp_pm_addr_send_ack_avoid_list(struct mptcp_sock *msk,
net/mptcp/pm.c
304
void mptcp_pm_addr_send_ack(struct mptcp_sock *msk)
net/mptcp/pm.c
309
int mptcp_pm_mp_prio_send_ack(struct mptcp_sock *msk,
net/mptcp/pm.c
342
static unsigned int mptcp_adjust_add_addr_timeout(struct mptcp_sock *msk)
net/mptcp/pm.c
380
struct mptcp_sock *msk = entry->sock;
net/mptcp/pm.c
435
bool mptcp_pm_announced_alloc(struct mptcp_sock *msk,
net/mptcp/pm.c
472
static void mptcp_pm_free_announced_list(struct mptcp_sock *msk)
net/mptcp/pm.c
493
int mptcp_pm_announce_addr(struct mptcp_sock *msk,
net/mptcp/pm.c
521
int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list)
net/mptcp/pm.c
542
void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side)
net/mptcp/pm.c
552
bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk)
net/mptcp/pm.c
592
static bool mptcp_pm_schedule_work(struct mptcp_sock *msk,
net/mptcp/pm.c
605
void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk)
net/mptcp/pm.c
632
void mptcp_pm_connection_closed(struct mptcp_sock *msk)
net/mptcp/pm.c
640
void mptcp_pm_subflow_established(struct mptcp_sock *msk)
net/mptcp/pm.c
657
void mptcp_pm_subflow_check_next(struct mptcp_sock *msk,
net/mptcp/pm.c
695
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/pm.c
729
void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk,
net/mptcp/pm.c
751
static void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk)
net/mptcp/pm.c
759
static void mptcp_pm_rm_addr_or_subflow(struct mptcp_sock *msk,
net/mptcp/pm.c
822
static void mptcp_pm_rm_addr_recv(struct mptcp_sock *msk)
net/mptcp/pm.c
827
void mptcp_pm_rm_subflow(struct mptcp_sock *msk,
net/mptcp/pm.c
833
void mptcp_pm_rm_addr_received(struct mptcp_sock *msk,
net/mptcp/pm.c
856
struct mptcp_sock *msk;
net/mptcp/pm.c
869
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/pm.c
909
bool mptcp_pm_add_addr_signal(struct mptcp_sock *msk, int *size, int remaining,
net/mptcp/pm.c
996
bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
net/mptcp/pm_kernel.c
1056
static void mptcp_pm_remove_announced(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
122
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
1274
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
1467
static void mptcp_pm_nl_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1488
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
150
select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
1572
bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
1586
void __mptcp_pm_kernel_worker(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
181
fill_remote_addr(struct mptcp_sock *msk, struct mptcp_addr_info *local,
net/mptcp/pm_kernel.c
203
fill_remote_addresses_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
253
fill_remote_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *local,
net/mptcp/pm_kernel.c
293
static u8 mptcp_endp_get_local_id(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
300
static void mptcp_mpc_endpoint_setup(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
333
static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
41
pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
441
static void mptcp_pm_nl_fully_established(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
446
static void mptcp_pm_nl_subflow_established(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
452
fill_local_addresses_vec_fullmesh(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
507
fill_local_laminar_endp(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
51
u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
567
fill_local_addresses_vec_c_flag(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
59
u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
606
fill_local_address_any(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
631
fill_local_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *remote,
net/mptcp/pm_kernel.c
657
static void mptcp_pm_nl_add_addr_received(struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
67
u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
706
void mptcp_pm_nl_rm_addr(struct mptcp_sock *msk, u8 rm_id)
net/mptcp/pm_kernel.c
75
u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
83
u8 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
91
u8 mptcp_pm_get_limit_extra_subflows(const struct mptcp_sock *msk)
net/mptcp/pm_kernel.c
918
int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk,
net/mptcp/pm_kernel.c
947
bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc)
net/mptcp/pm_kernel.c
964
struct mptcp_sock *msk;
net/mptcp/pm_kernel.c
99
static bool has_subflow_daddr(const 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
15
void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk)
net/mptcp/pm_userspace.c
151
bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
165
static struct mptcp_sock *mptcp_userspace_pm_get_sock(const struct genl_info *info)
net/mptcp/pm_userspace.c
167
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
193
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
249
static int mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk)
net/mptcp/pm_userspace.c
280
void mptcp_pm_remove_addr_entry(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
303
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
31
mptcp_userspace_pm_lookup_addr(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
366
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
435
static struct sock *mptcp_nl_find_ssk(struct mptcp_sock *msk,
net/mptcp/pm_userspace.c
486
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
566
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
634
struct mptcp_sock *msk;
net/mptcp/pm_userspace.c
671
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
103
static int __mptcp_socket_create(struct mptcp_sock *msk)
net/mptcp/protocol.c
1045
static bool mptcp_frag_can_collapse_to(const struct mptcp_sock *msk,
net/mptcp/protocol.c
1074
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1149
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1179
mptcp_carve_data_frag(const struct mptcp_sock *msk, struct page_frag *pfrag,
net/mptcp/protocol.c
1206
static size_t mptcp_check_allowed_size(const struct mptcp_sock *msk,
net/mptcp/protocol.c
1292
static void mptcp_update_infinite_map(struct mptcp_sock *msk,
net/mptcp/protocol.c
1319
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
1505
struct sock *mptcp_subflow_get_send(struct mptcp_sock *msk)
net/mptcp/protocol.c
1587
static void mptcp_update_post_push(struct mptcp_sock *msk,
net/mptcp/protocol.c
1626
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1670
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1737
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1808
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1881
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
1898
static void mptcp_rps_record_subflows(const struct mptcp_sock *msk)
net/mptcp/protocol.c
1914
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
2052
static void mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied);
net/mptcp/protocol.c
2070
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
210
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2133
static void mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk)
net/mptcp/protocol.c
2152
static void mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied)
net/mptcp/protocol.c
2209
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2237
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2258
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2288
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2310
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2422
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
243
static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb)
net/mptcp/protocol.c
2452
struct sock *mptcp_subflow_get_retrans(struct mptcp_sock *msk)
net/mptcp/protocol.c
2491
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2550
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2576
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2706
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2739
static void mptcp_check_fastclose(struct mptcp_sock *msk)
net/mptcp/protocol.c
2791
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2900
void mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout)
net/mptcp/protocol.c
2919
static void mptcp_mp_fail_no_response(struct mptcp_sock *msk)
net/mptcp/protocol.c
2937
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2956
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
2991
struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work);
net/mptcp/protocol.c
3040
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3123
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3133
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3227
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3251
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3266
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3320
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3425
static void mptcp_destroy_common(struct mptcp_sock *msk)
net/mptcp/protocol.c
3449
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3566
struct mptcp_sock *msk;
net/mptcp/protocol.c
3640
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3672
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
379
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3798
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
38
struct mptcp_sock msk;
net/mptcp/protocol.c
3810
struct mptcp_sock *msk;
net/mptcp/protocol.c
3859
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/protocol.c
3932
static int mptcp_ioctl_outq(const struct mptcp_sock *msk, u64 v)
net/mptcp/protocol.c
3963
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
3998
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4100
.obj_size = sizeof(struct mptcp_sock),
net/mptcp/protocol.c
4107
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4134
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4175
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4238
struct mptcp_sock *msk = mptcp_sk(sock->sk);
net/mptcp/protocol.c
4314
static __poll_t mptcp_check_writeable(struct mptcp_sock *msk)
net/mptcp/protocol.c
4333
struct mptcp_sock *msk;
net/mptcp/protocol.c
4380
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
4405
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
441
static void mptcp_shutdown_subflows(struct mptcp_sock *msk)
net/mptcp/protocol.c
458
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
467
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
491
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
564
static void mptcp_send_ack(struct mptcp_sock *msk)
net/mptcp/protocol.c
59
static u64 mptcp_wnd_end(const struct mptcp_sock *msk)
net/mptcp/protocol.c
595
static void mptcp_cleanup_rbuf(struct mptcp_sock *msk, int copied)
net/mptcp/protocol.c
616
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
662
static void mptcp_dss_corruption(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
674
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
712
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
787
static bool __mptcp_ofo_queue(struct mptcp_sock *msk)
net/mptcp/protocol.c
866
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
876
static bool move_skbs_to_msk(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
896
static void mptcp_rcv_rtt_update(struct mptcp_sock *msk,
net/mptcp/protocol.c
925
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.c
946
static void mptcp_subflow_joined(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
953
static bool __mptcp_finish_join(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/protocol.c
978
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
1080
struct mptcp_sock *msk);
net/mptcp/protocol.h
1082
struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token);
net/mptcp/protocol.h
1083
struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot,
net/mptcp/protocol.h
1085
void mptcp_token_destroy(struct mptcp_sock *msk);
net/mptcp/protocol.h
1093
void mptcp_pm_data_init(struct mptcp_sock *msk);
net/mptcp/protocol.h
1094
void mptcp_pm_data_reset(struct mptcp_sock *msk);
net/mptcp/protocol.h
1095
void mptcp_pm_destroy(struct mptcp_sock *msk);
net/mptcp/protocol.h
1104
void mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk);
net/mptcp/protocol.h
1105
void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side);
net/mptcp/protocol.h
1106
void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk);
net/mptcp/protocol.h
1107
bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk);
net/mptcp/protocol.h
1108
void mptcp_pm_connection_closed(struct mptcp_sock *msk);
net/mptcp/protocol.h
1109
void mptcp_pm_subflow_established(struct mptcp_sock *msk);
net/mptcp/protocol.h
1110
bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk);
net/mptcp/protocol.h
1111
void mptcp_pm_subflow_check_next(struct mptcp_sock *msk,
net/mptcp/protocol.h
1115
void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk,
net/mptcp/protocol.h
1117
void mptcp_pm_send_ack(struct mptcp_sock *msk,
net/mptcp/protocol.h
1120
void mptcp_pm_addr_send_ack(struct mptcp_sock *msk);
net/mptcp/protocol.h
1121
void mptcp_pm_nl_rm_addr(struct mptcp_sock *msk, u8 rm_id);
net/mptcp/protocol.h
1122
void mptcp_pm_rm_subflow(struct mptcp_sock *msk,
net/mptcp/protocol.h
1124
void mptcp_pm_rm_addr_received(struct mptcp_sock *msk,
net/mptcp/protocol.h
1128
int mptcp_pm_mp_prio_send_ack(struct mptcp_sock *msk,
net/mptcp/protocol.h
1132
bool mptcp_pm_announced_alloc(struct mptcp_sock *msk,
net/mptcp/protocol.h
1134
bool mptcp_pm_announced_remove(struct mptcp_sock *msk,
net/mptcp/protocol.h
1136
bool mptcp_pm_announced_has_ssk(struct mptcp_sock *msk, const struct sock *ssk);
net/mptcp/protocol.h
1137
bool mptcp_pm_has_subflow_saddr(const struct mptcp_sock *msk,
net/mptcp/protocol.h
1143
int mptcp_pm_announce_addr(struct mptcp_sock *msk,
net/mptcp/protocol.h
1146
int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list);
net/mptcp/protocol.h
1147
void mptcp_pm_remove_addr_entry(struct mptcp_sock *msk,
net/mptcp/protocol.h
1159
void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk);
net/mptcp/protocol.h
1161
void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk,
net/mptcp/protocol.h
1164
void mptcp_event_addr_removed(const struct mptcp_sock *msk, u8 id);
net/mptcp/protocol.h
1167
bool mptcp_userspace_pm_active(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1175
static inline bool mptcp_pm_should_add_signal(struct mptcp_sock *msk)
net/mptcp/protocol.h
1181
static inline bool mptcp_pm_should_add_signal_addr(struct mptcp_sock *msk)
net/mptcp/protocol.h
1186
static inline bool mptcp_pm_should_add_signal_echo(struct mptcp_sock *msk)
net/mptcp/protocol.h
1191
static inline bool mptcp_pm_should_rm_signal(struct mptcp_sock *msk)
net/mptcp/protocol.h
1196
static inline bool mptcp_pm_is_userspace(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1201
static inline bool mptcp_pm_is_kernel(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1206
bool mptcp_pm_add_addr_signal(struct mptcp_sock *msk, int *size, int remaining,
net/mptcp/protocol.h
1209
bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
net/mptcp/protocol.h
1211
int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
net/mptcp/protocol.h
1212
int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk,
net/mptcp/protocol.h
1214
int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk,
net/mptcp/protocol.h
1216
bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
net/mptcp/protocol.h
1217
bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
net/mptcp/protocol.h
1218
bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
net/mptcp/protocol.h
1240
void mptcp_pm_worker(struct mptcp_sock *msk);
net/mptcp/protocol.h
1241
void __mptcp_pm_kernel_worker(struct mptcp_sock *msk);
net/mptcp/protocol.h
1242
u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1243
u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1244
u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1245
u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1246
u8 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1247
u8 mptcp_pm_get_limit_extra_subflows(const struct mptcp_sock *msk);
net/mptcp/protocol.h
1250
static inline void __mptcp_pm_close_subflow(struct mptcp_sock *msk)
net/mptcp/protocol.h
1256
static inline void mptcp_pm_close_subflow(struct mptcp_sock *msk)
net/mptcp/protocol.h
1263
static inline bool mptcp_pm_add_addr_c_flag_case(struct mptcp_sock *msk)
net/mptcp/protocol.h
1271
void mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk);
net/mptcp/protocol.h
1280
static inline bool __mptcp_check_fallback(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1288
struct mptcp_sock *msk = mptcp_sk(subflow->conn);
net/mptcp/protocol.h
1293
static inline bool __mptcp_has_initial_subflow(const struct mptcp_sock *msk)
net/mptcp/protocol.h
1302
bool __mptcp_try_fallback(struct mptcp_sock *msk, int fb_mib);
net/mptcp/protocol.h
1308
struct mptcp_sock *msk;
net/mptcp/protocol.h
1327
static inline void mptcp_early_fallback(struct mptcp_sock *msk,
net/mptcp/protocol.h
392
static inline void msk_owned_by_me(const struct mptcp_sock *msk)
net/mptcp/protocol.h
408
container_of_const(_ptr, struct mptcp_sock, sk.icsk_inet.sk); \
net/mptcp/protocol.h
412
#define mptcp_sk(ptr) container_of_const(ptr, struct mptcp_sock, sk.icsk_inet.sk)
net/mptcp/protocol.h
434
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
439
static inline void mptcp_init_rtt_est(struct mptcp_sock *msk)
net/mptcp/protocol.h
449
static inline u32 mptcp_rtt_us_est(const struct mptcp_sock *msk)
net/mptcp/protocol.h
462
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
472
const struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
485
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/protocol.h
517
struct mptcp_sock *msk;
net/mptcp/protocol.h
808
void __mptcp_subflow_fully_established(struct mptcp_sock *msk,
net/mptcp/protocol.h
823
struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk);
net/mptcp/protocol.h
849
int mptcp_init_sched(struct mptcp_sock *msk,
net/mptcp/protocol.h
851
void mptcp_release_sched(struct mptcp_sock *msk);
net/mptcp/protocol.h
854
struct sock *mptcp_subflow_get_send(struct mptcp_sock *msk);
net/mptcp/protocol.h
855
struct sock *mptcp_subflow_get_retrans(struct mptcp_sock *msk);
net/mptcp/protocol.h
856
int mptcp_sched_get_send(struct mptcp_sock *msk);
net/mptcp/protocol.h
857
int mptcp_sched_get_retrans(struct mptcp_sock *msk);
net/mptcp/protocol.h
859
static inline u64 mptcp_data_avail(const struct mptcp_sock *msk)
net/mptcp/protocol.h
927
void mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout);
net/mptcp/protocol.h
980
bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit);
net/mptcp/protocol.h
981
static inline bool mptcp_data_fin_enabled(const struct mptcp_sock *msk)
net/mptcp/protocol.h
998
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
1034
static int mptcp_getsockopt_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen)
net/mptcp/sockopt.c
1118
static int mptcp_getsockopt_tcpinfo(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
1210
static int mptcp_getsockopt_subflow_addrs(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
129
static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
1308
static int mptcp_getsockopt_full_info(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
1382
static int mptcp_put_int_option(struct mptcp_sock *msk, char __user *optval,
net/mptcp/sockopt.c
1411
static int mptcp_getsockopt_sol_tcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
144
static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
1457
static int mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1482
static int mptcp_getsockopt_v6(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1502
static int mptcp_getsockopt_sol_mptcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
1522
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/sockopt.c
153
static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
1550
static void sync_socket_options(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/sockopt.c
1606
void mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk)
net/mptcp/sockopt.c
178
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
211
static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk,
net/mptcp/sockopt.c
259
static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval,
net/mptcp/sockopt.c
300
static int mptcp_setsockopt_sol_socket(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
397
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
592
static int mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock *msk, sockptr_t optval,
net/mptcp/sockopt.c
635
static int __mptcp_setsockopt_set_val(struct mptcp_sock *msk, int max,
net/mptcp/sockopt.c
660
static int __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
680
static int __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock *msk, int val)
net/mptcp/sockopt.c
699
static int mptcp_setsockopt_sol_ip_set(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
745
static int mptcp_setsockopt_v4_set_tos(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
76
static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val)
net/mptcp/sockopt.c
773
static int mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
789
static int mptcp_setsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname,
net/mptcp/sockopt.c
811
static int mptcp_setsockopt_all_sf(struct mptcp_sock *msk, int level,
net/mptcp/sockopt.c
833
static int mptcp_setsockopt_sol_tcp(struct mptcp_sock *msk, int optname,
net/mptcp/sockopt.c
910
struct mptcp_sock *msk = mptcp_sk(sk);
net/mptcp/sockopt.c
945
static int mptcp_getsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname,
net/mptcp/sockopt.c
971
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)
