| /openbmc/linux/net/mptcp/ |
| H A D | protocol.h | 258 struct mptcp_sock { struct
345 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me() argument
350 #define mptcp_sk(ptr) container_of_const(ptr, struct mptcp_sock, sk.icsk_inet.sk)
372 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head()
379 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next()
389 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail()
402 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head()
434 struct mptcp_sock *msk;
633 void __mptcp_subflow_fully_established(struct mptcp_sock *msk,
648 struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk);
[all …]
|
| H A D | pm.c | 17 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr()
45 int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) in mptcp_pm_remove_addr()
66 void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side) in mptcp_pm_new_connection()
76 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) in mptcp_pm_allow_new_subflow()
115 static bool mptcp_pm_schedule_work(struct mptcp_sock *msk, in mptcp_pm_schedule_work()
128 void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk) in mptcp_pm_fully_established()
155 void mptcp_pm_connection_closed(struct mptcp_sock *msk) in mptcp_pm_connection_closed()
160 void mptcp_pm_subflow_established(struct mptcp_sock *msk) in mptcp_pm_subflow_established()
177 void mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct sock *ssk, in mptcp_pm_subflow_check_next()
213 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_pm_add_addr_received()
[all …]
|
| H 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()
56 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); in build_msk()
70 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic()
71 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_msk_basic()
92 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept()
111 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed()
112 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_destroyed()
|
| H 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()
70 static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_sync_intval()
123 static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_intval()
138 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) in mptcp_so_incoming_cpu()
147 static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) in mptcp_setsockopt_sol_socket_tstamp()
172 static int mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_sol_socket_int()
205 static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk, in mptcp_setsockopt_sol_socket_timestamping()
249 static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval, in mptcp_setsockopt_sol_socket_linger()
[all …]
|
| H 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()
|
| H A D | pm_netlink.c | 31 struct mptcp_sock *sock;
57 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk()
156 const struct mptcp_sock *msk, in select_local_address()
182 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk, in select_signal_address()
210 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_signal_max()
218 unsigned int mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_accept_max()
226 unsigned int mptcp_pm_get_subflows_max(const struct mptcp_sock *msk) in mptcp_pm_get_subflows_max()
234 unsigned int mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk) in mptcp_pm_get_local_addr_max()
242 bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk) in mptcp_pm_nl_check_work_pending()
256 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, in mptcp_lookup_anno_list_by_saddr()
[all …]
|
| H A D | protocol.c | 34 struct mptcp_sock msk;
53 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) in mptcp_wnd_end()
68 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create()
98 struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk) in __mptcp_nmpc_sk()
160 static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, in mptcp_ooo_try_coalesce()
178 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_uncharge()
211 static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) in mptcp_data_queue_ofo()
324 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_schedule()
340 static bool __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, in __mptcp_move_skb()
419 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin_ack()
[all …]
|
| H A D | sched.c | 19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk, in mptcp_sched_default_get_subflow()
86 int mptcp_init_sched(struct mptcp_sock *msk, in mptcp_init_sched()
104 void mptcp_release_sched(struct mptcp_sock *msk) in mptcp_release_sched()
124 int mptcp_sched_get_send(struct mptcp_sock *msk) in mptcp_sched_get_send()
153 int mptcp_sched_get_retrans(struct mptcp_sock *msk) in mptcp_sched_get_retrans()
|
| H A D | pm_userspace.c | 10 void mptcp_free_local_addr_list(struct mptcp_sock *msk) in mptcp_free_local_addr_list()
28 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_append_new_local_addr()
89 static int mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_delete_local_addr()
111 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id) in mptcp_userspace_pm_lookup_addr_by_id()
122 int mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_flags_and_ifindex_by_id()
139 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_local_id()
168 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, in mptcp_userspace_pm_is_backup()
191 struct mptcp_sock *msk; in mptcp_nl_cmd_announce()
252 static int mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk, in mptcp_userspace_pm_remove_id_zero_address()
292 struct mptcp_sock *msk; in mptcp_nl_cmd_remove()
[all …]
|
| H A D | subflow.c | 62 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow()
73 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac()
85 static struct mptcp_sock *subflow_token_join_request(struct request_sock *req) in subflow_token_join_request()
88 struct mptcp_sock *msk; in subflow_token_join_request()
120 static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_sport()
432 static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_dport()
440 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_sync_state()
459 static void subflow_set_remote_key(struct mptcp_sock *msk, in subflow_set_remote_key()
484 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_propagate_state()
510 struct mptcp_sock *msk; in subflow_finish_connect()
[all …]
|
| H 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()
925 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established()
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()
1079 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) in mptcp_update_rcv_data_fin()
[all …]
|
| H A D | mptcp_diag.c | 32 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one()
159 struct mptcp_sock *msk; in mptcp_diag_dump()
203 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_diag_get_info()
|
| H A D | bpf.c | 15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) in bpf_mptcp_sock_from_subflow()
|
| H 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()
|
| H A D | syncookies.c | 97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state()
|
| /openbmc/linux/include/net/ |
| H A D | mptcp.h | 16 struct mptcp_sock;
109 int (*get_subflow)(struct mptcp_sock *msk,
116 void (*init)(struct mptcp_sock *msk);
117 void (*release)(struct mptcp_sock *msk);
151 void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
318 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
320 static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; } in bpf_mptcp_sock_from_subflow()
324 struct mptcp_sock { }; struct
|
| /openbmc/linux/tools/testing/selftests/bpf/progs/ |
| H 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()
|
| /openbmc/linux/tools/include/linux/ |
| H A D | btf_ids.h | 192 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
| /openbmc/linux/include/linux/ |
| H A D | btf_ids.h | 242 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
| /openbmc/linux/tools/testing/selftests/bpf/ |
| H A D | bpf_tcp_helpers.h | 233 struct mptcp_sock { struct
|
| /openbmc/linux/tools/testing/selftests/bpf/prog_tests/ |
| H A D | mptcp.c | 159 struct mptcp_sock *sock_skel; in run_test()
|
| /openbmc/linux/net/core/ |
| H A D | filter.c | 11778 BTF_TYPE_EMIT(struct mptcp_sock); in BPF_CALL_1()
|
| /openbmc/linux/ |
| H A D | opengrok0.0.log | [all...] |