/linux-6.1.9/net/mptcp/ |
D | protocol.h | 250 struct mptcp_sock { struct 311 struct mptcp_sock *dl_next; argument 322 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me() 327 static inline struct mptcp_sock *mptcp_sk(const struct sock *sk) in mptcp_sk() 329 return (struct mptcp_sock *)sk; in mptcp_sk() 347 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head() 354 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next() 364 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail() 377 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head() 408 struct mptcp_sock *msk; [all …]
|
D | pm.c | 17 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr() 44 int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) in mptcp_pm_remove_addr() 62 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) in mptcp_pm_remove_subflow() 74 void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side) in mptcp_pm_new_connection() 84 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) in mptcp_pm_allow_new_subflow() 116 static bool mptcp_pm_schedule_work(struct mptcp_sock *msk, in mptcp_pm_schedule_work() 129 void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk, gfp_t gfp) in mptcp_pm_fully_established() 156 void mptcp_pm_connection_closed(struct mptcp_sock *msk) in mptcp_pm_connection_closed() 161 void mptcp_pm_subflow_established(struct mptcp_sock *msk) in mptcp_pm_subflow_established() 178 void mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct sock *ssk, in mptcp_pm_subflow_check_next() [all …]
|
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() 67 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() 68 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_msk_basic() 89 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept() 108 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed() 109 struct mptcp_sock *null_msk = NULL; in mptcp_token_test_destroyed()
|
D | sockopt.c | 19 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback() 50 static void sockopt_seq_inc(struct mptcp_sock *msk) in sockopt_seq_inc() 57 static int mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval, in mptcp_get_int_option() 69 static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_sync_intval() 121 static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_intval() 136 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) in mptcp_so_incoming_cpu() 145 static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) in mptcp_setsockopt_sol_socket_tstamp() 170 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 …]
|
D | token.c | 67 static struct mptcp_sock * 154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() 190 struct mptcp_sock *msk) in mptcp_token_accept() 210 struct mptcp_sock *msk; in mptcp_token_exists() 242 struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token) in mptcp_token_get_sock() 246 struct mptcp_sock *msk; in mptcp_token_get_sock() 293 struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot, in mptcp_token_iter_next() 296 struct mptcp_sock *ret = NULL; in mptcp_token_iter_next() 371 void mptcp_token_destroy(struct mptcp_sock *msk) in mptcp_token_destroy() 374 struct mptcp_sock *pos; in mptcp_token_destroy()
|
D | protocol.c | 34 struct mptcp_sock msk; 65 struct socket *__mptcp_nmpc_socket(const struct mptcp_sock *msk) in __mptcp_nmpc_socket() 74 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) in mptcp_wnd_end() 103 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create() 165 static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, in mptcp_ooo_try_coalesce() 183 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_uncharge() 216 static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) in mptcp_data_queue_ofo() 329 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_schedule() 345 static bool __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, in __mptcp_move_skb() 421 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin_ack() [all …]
|
D | pm_netlink.c | 29 struct mptcp_sock *sock; 56 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk() 153 const struct mptcp_sock *msk) in select_local_address() 186 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 …]
|
D | pm_userspace.c | 10 void mptcp_free_local_addr_list(struct mptcp_sock *msk) in mptcp_free_local_addr_list() 28 int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_append_new_local_addr() 81 int mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_flags_and_ifindex_by_id() 106 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_local_id() 129 struct mptcp_sock *msk; in mptcp_nl_cmd_announce() 192 struct mptcp_sock *msk; in mptcp_nl_cmd_remove() 255 struct mptcp_sock *msk; in mptcp_nl_cmd_sf_create() 315 static struct sock *mptcp_nl_find_ssk(struct mptcp_sock *msk, in mptcp_nl_find_ssk() 370 struct mptcp_sock *msk; in mptcp_nl_cmd_sf_destroy() 441 struct mptcp_sock *msk; in mptcp_userspace_pm_set_flags()
|
D | subflow.c | 61 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow() 72 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac() 84 static struct mptcp_sock *subflow_token_join_request(struct request_sock *req) in subflow_token_join_request() 87 struct mptcp_sock *msk; in subflow_token_join_request() 118 static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_sport() 371 static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_dport() 495 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in subflow_chk_local_id() 618 struct mptcp_sock *msk; in subflow_hmac_valid() 669 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_subflow_fully_established() 793 struct mptcp_sock *owner; in subflow_syn_recv_sock() [all …]
|
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()
|
D | options.c | 444 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp() 558 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() 652 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() 704 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr() 779 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose() 824 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options() 919 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established() 1020 static void ack_update_msk(struct mptcp_sock *msk, in ack_update_msk() 1061 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) in mptcp_update_rcv_data_fin() 1078 static bool add_addr_hmac_valid(struct mptcp_sock *msk, in add_addr_hmac_valid() [all …]
|
D | bpf.c | 15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) in bpf_mptcp_sock_from_subflow()
|
D | syncookies.c | 97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state()
|
/linux-6.1.9/include/net/ |
D | mptcp.h | 16 struct mptcp_sock; 130 void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info); 297 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk); 299 static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; } in bpf_mptcp_sock_from_subflow() 303 struct mptcp_sock { }; struct
|
/linux-6.1.9/tools/testing/selftests/bpf/progs/ |
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-6.1.9/tools/include/linux/ |
D | btf_ids.h | 181 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
/linux-6.1.9/tools/testing/selftests/bpf/prog_tests/ |
D | mptcp.c | 97 struct mptcp_sock *sock_skel; in run_test()
|
/linux-6.1.9/include/linux/ |
D | btf_ids.h | 242 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
/linux-6.1.9/tools/testing/selftests/bpf/ |
D | bpf_tcp_helpers.h | 233 struct mptcp_sock { struct
|
/linux-6.1.9/net/core/ |
D | filter.c | 11492 BTF_TYPE_EMIT(struct mptcp_sock); in BPF_CALL_1()
|