| /linux/net/mptcp/ |
| A D | protocol.h | 264 struct mptcp_sock { struct
407 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head()
414 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next()
424 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail()
437 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head()
469 struct mptcp_sock *msk;
746 int mptcp_init_sched(struct mptcp_sock *msk,
887 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_stream_memory_free()
971 struct mptcp_sock *msk);
1025 mptcp_pm_del_add_timer(struct mptcp_sock *msk,
[all …]
|
| A D | pm.c | 16 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr()
75 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) in mptcp_pm_allow_new_subflow()
154 void mptcp_pm_connection_closed(struct mptcp_sock *msk) in mptcp_pm_connection_closed()
212 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_pm_add_addr_received()
243 void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk, in mptcp_pm_add_addr_echoed()
258 void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk) in mptcp_pm_add_addr_send_ack()
266 void mptcp_pm_rm_addr_received(struct mptcp_sock *msk, in mptcp_pm_rm_addr_received()
289 struct mptcp_sock *msk; in mptcp_pm_mp_prio_received()
302 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_pm_mp_fail_received()
500 void mptcp_pm_data_reset(struct mptcp_sock *msk) in mptcp_pm_data_reset()
[all …]
|
| A D | token_test.c | 21 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_req_basic()
52 static struct mptcp_sock *build_msk(struct kunit *test) in build_msk()
54 struct mptcp_sock *msk; in build_msk()
57 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); in build_msk()
75 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic()
76 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_msk_basic()
97 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept()
116 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed()
117 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_destroyed()
|
| A D | sockopt.c | 20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback()
51 static void sockopt_seq_inc(struct mptcp_sock *msk) in sockopt_seq_inc()
58 static int mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval, in mptcp_get_int_option()
138 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) in mptcp_so_incoming_cpu()
387 static int mptcp_setsockopt_v6(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_v6()
625 static int __mptcp_setsockopt_set_val(struct mptcp_sock *msk, int max, in __mptcp_setsockopt_set_val()
763 static int mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_v4()
801 static int mptcp_setsockopt_sol_tcp(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_sol_tcp()
873 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_setsockopt()
1414 static int mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname, in mptcp_getsockopt_v4()
[all …]
|
| A D | token.c | 67 static struct mptcp_sock *
154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect()
192 struct mptcp_sock *msk) in mptcp_token_accept()
214 struct mptcp_sock *msk; in mptcp_token_exists()
246 struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token) in mptcp_token_get_sock()
250 struct mptcp_sock *msk; in mptcp_token_get_sock()
297 struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot, in mptcp_token_iter_next()
300 struct mptcp_sock *ret = NULL; in mptcp_token_iter_next()
375 void mptcp_token_destroy(struct mptcp_sock *msk) in mptcp_token_destroy()
379 struct mptcp_sock *pos; in mptcp_token_destroy()
|
| A D | pm_netlink.c | 26 struct mptcp_sock *sock;
151 const struct mptcp_sock *msk, in select_local_address()
294 struct mptcp_sock *msk = entry->sock; in mptcp_pm_add_timer()
1351 struct mptcp_sock *msk; in mptcp_nl_add_subflow_or_signal_addr()
1505 struct mptcp_sock *msk; in mptcp_nl_remove_subflow_and_signal_addr()
1556 struct mptcp_sock *msk; in mptcp_nl_remove_id_zero_address()
1698 struct mptcp_sock *msk; in mptcp_nl_flush_addrs_list()
1989 struct mptcp_sock *msk; in mptcp_nl_set_flags()
2135 const struct mptcp_sock *msk, in mptcp_event_put_token_and_ssk()
2175 const struct mptcp_sock *msk, in mptcp_event_sub_closed()
[all …]
|
| A D | protocol.c | 34 struct mptcp_sock msk;
176 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_uncharge()
322 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_schedule()
418 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin_ack()
427 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin_ack()
450 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin()
575 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin()
2771 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); in mptcp_worker()
3307 struct mptcp_sock *msk; in mptcp_sk_clone_init()
3591 struct mptcp_sock *msk; in mptcp_finish_connect()
[all …]
|
| A D | sched.c | 19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk, in mptcp_sched_default_get_subflow()
108 int mptcp_init_sched(struct mptcp_sock *msk, in mptcp_init_sched()
126 void mptcp_release_sched(struct mptcp_sock *msk) in mptcp_release_sched()
146 int mptcp_sched_get_send(struct mptcp_sock *msk) in mptcp_sched_get_send()
175 int mptcp_sched_get_retrans(struct mptcp_sock *msk) in mptcp_sched_get_retrans()
|
| A D | pm_userspace.c | 11 void mptcp_free_local_addr_list(struct mptcp_sock *msk) in mptcp_free_local_addr_list()
123 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_local_id()
152 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, in mptcp_userspace_pm_is_backup()
175 struct mptcp_sock *msk; in mptcp_pm_nl_announce_doit()
276 struct mptcp_sock *msk; in mptcp_pm_nl_remove_doit()
345 struct mptcp_sock *msk; in mptcp_pm_nl_subflow_create_doit()
421 static struct sock *mptcp_nl_find_ssk(struct mptcp_sock *msk, in mptcp_nl_find_ssk()
476 struct mptcp_sock *msk; in mptcp_pm_nl_subflow_destroy_doit()
567 struct mptcp_sock *msk; in mptcp_userspace_pm_set_flags()
637 struct mptcp_sock *msk; in mptcp_userspace_pm_dump_addr()
[all …]
|
| A D | subflow.c | 72 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac()
88 struct mptcp_sock *msk; in subflow_token_join_request()
459 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_sync_state()
503 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_propagate_state()
529 struct mptcp_sock *msk; in subflow_finish_connect()
753 struct mptcp_sock *msk; in subflow_hmac_valid()
822 struct mptcp_sock *owner; in subflow_syn_recv_sock()
1099 struct mptcp_sock *msk) in get_mapping_status()
1330 struct mptcp_sock *msk; in subflow_check_data_avail()
1483 struct mptcp_sock *msk; in subflow_data_ready()
[all …]
|
| A D | options.c | 449 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp()
562 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss()
655 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr()
710 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr()
785 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose()
830 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options()
1032 static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) in __mptcp_snd_una_update()
1038 static void ack_update_msk(struct mptcp_sock *msk, in ack_update_msk()
1097 static bool add_addr_hmac_valid(struct mptcp_sock *msk, in add_addr_hmac_valid()
1119 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_incoming_options()
[all …]
|
| A D | mptcp_diag.c | 31 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one()
158 struct mptcp_sock *msk; in mptcp_diag_dump()
202 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_diag_get_info()
|
| A D | bpf.c | 15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) in bpf_mptcp_sock_from_subflow()
|
| A D | fastopen.c | 62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_fastopen_gen_msk_ackseq()
|
| A D | syncookies.c | 97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state()
|
| /linux/include/net/ |
| A D | mptcp.h | 16 struct mptcp_sock;
112 int (*get_subflow)(struct mptcp_sock *msk,
119 void (*init)(struct mptcp_sock *msk);
120 void (*release)(struct mptcp_sock *msk);
154 void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
325 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
327 static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; } in bpf_mptcp_sock_from_subflow()
331 struct mptcp_sock { }; struct
|
| /linux/tools/testing/selftests/bpf/progs/ |
| A D | mptcp_sock.c | 32 struct mptcp_sock *msk; in _sockops()
81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk, in BPF_PROG()
|
| /linux/tools/include/linux/ |
| A D | btf_ids.h | 192 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
| /linux/include/linux/ |
| A D | btf_ids.h | 257 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
| /linux/tools/testing/selftests/bpf/prog_tests/ |
| A D | mptcp.c | 170 struct mptcp_sock *sock_skel; in run_test()
|
| /linux/net/core/ |
| A D | filter.c | 11833 BTF_TYPE_EMIT(struct mptcp_sock); in BPF_CALL_1()
|