Home
last modified time | relevance | path

Searched refs:mptcp_sock (Results 1 – 15 of 15) sorted by relevance

/linux/net/mptcp/
H A Dpm.c21 struct mptcp_sock *sock;
109 static bool mptcp_pm_is_init_remote_addr(struct mptcp_sock *msk, in mptcp_pm_is_init_remote_addr()
118 bool mptcp_pm_has_subflow_saddr(const struct mptcp_sock *msk, in mptcp_pm_has_subflow_saddr()
137 mptcp_pm_announced_lookup(const struct mptcp_sock *msk, in mptcp_pm_announced_lookup()
153 mptcp_pm_announced_del_timer(struct mptcp_sock *msk, in mptcp_pm_announced_del_timer()
186 bool mptcp_pm_announced_remove(struct mptcp_sock *msk, in mptcp_pm_announced_remove()
199 bool mptcp_pm_announced_has_ssk(struct mptcp_sock *msk, const struct sock *ssk) in mptcp_pm_announced_has_ssk()
220 static void __mptcp_pm_send_ack(struct mptcp_sock *msk, in __mptcp_pm_send_ack()
241 void mptcp_pm_send_ack(struct mptcp_sock *msk, in mptcp_pm_send_ack()
263 static void mptcp_pm_add_addr_send_ack(struct mptcp_sock *ms
[all...]
H A Dtoken_test.c21 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()
H A Dpm_userspace.c15 void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk) in mptcp_userspace_pm_free_local_addr_list()
31 mptcp_userspace_pm_lookup_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_lookup_addr()
43 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_append_new_local_addr()
112 static int mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_delete_local_addr()
132 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id)
143 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_local_id()
165 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, in mptcp_userspace_pm_is_backup()
179 static struct mptcp_sock *mptcp_userspace_pm_get_sock(const struct genl_info *info) in mptcp_userspace_pm_get_sock()
181 struct mptcp_sock *msk; in mptcp_userspace_pm_get_sock()
207 struct mptcp_sock *ms in mptcp_pm_nl_announce_doit()
[all...]
H A Dsockopt.c20 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()
76 static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_sync_intval()
129 static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_intval()
144 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) in mptcp_so_incoming_cpu()
153 static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) in mptcp_setsockopt_sol_socket_tstamp()
178 static int mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_sol_socket_int()
211 static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk, in mptcp_setsockopt_sol_socket_timestamping()
259 static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval, in mptcp_setsockopt_sol_socket_linger()
[all …]
H A Dsched.c19 static int mptcp_sched_default_get_send(struct mptcp_sock *msk) in mptcp_sched_default_get_send()
31 static int mptcp_sched_default_get_retrans(struct mptcp_sock *msk)
130 int mptcp_init_sched(struct mptcp_sock *msk, in mptcp_init_sched()
148 void mptcp_release_sched(struct mptcp_sock *msk) in mptcp_release_sched()
168 int mptcp_sched_get_send(struct mptcp_sock *msk) in mptcp_sched_get_send()
195 int mptcp_sched_get_retrans(struct mptcp_sock *msk) in mptcp_sched_get_retrans()
H A Dpm_netlink.c291 bool mptcp_userspace_pm_active(const struct mptcp_sock *msk) in mptcp_userspace_pm_active()
346 const struct mptcp_sock *msk, in mptcp_event_put_token_and_ssk()
379 const struct mptcp_sock *msk, in mptcp_event_sub_established()
386 const struct mptcp_sock *msk, in mptcp_event_sub_closed()
408 const struct mptcp_sock *msk, in mptcp_event_created()
434 void mptcp_event_addr_removed(const struct mptcp_sock *msk, uint8_t id) in mptcp_event_addr_removed()
469 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_event_addr_announced()
572 void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk, in mptcp_event()
H A Doptions.c518 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp()
631 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss()
728 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr()
767 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr()
833 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose()
877 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options()
977 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established()
1086 static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) in __mptcp_snd_una_update()
1092 static void rwin_update(struct mptcp_sock *msk, struct sock *ssk, in rwin_update()
1118 static void ack_update_msk(struct mptcp_sock *ms in ack_update_msk()
[all...]
H A Dsubflow.c61 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()
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()
121 static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_sport()
449 static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_dport()
457 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_sync_state()
474 static void subflow_set_remote_key(struct mptcp_sock *msk, in subflow_set_remote_key()
502 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_propagate_state()
528 struct mptcp_sock *ms in subflow_finish_connect()
[all...]
H A Dbpf.c15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) in bpf_mptcp_sock_from_subflow()
/linux/include/net/
H A Dmptcp.h16 struct mptcp_sock;
105 int (*get_send)(struct mptcp_sock *msk);
106 int (*get_retrans)(struct mptcp_sock *msk);
112 void (*init)(struct mptcp_sock *msk);
113 void (*release)(struct mptcp_sock *msk);
125 void (*init)(struct mptcp_sock *msk);
126 void (*release)(struct mptcp_sock *msk);
160 void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
322 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
324 static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; } in bpf_mptcp_sock_from_subflow()
[all …]
/linux/tools/testing/selftests/bpf/progs/
H A Dmptcp_sock.c32 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/
H A Dbtf_ids.h256 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
/linux/include/trace/events/
H A Dmptcp.h214 struct mptcp_sock *msk = mptcp_sk(sk);
/linux/tools/testing/selftests/bpf/prog_tests/
H A Dmptcp.c159 struct mptcp_sock *sock_skel; in run_test()
/linux/net/core/
H A Dfilter.c12330 BTF_TYPE_EMIT(struct mptcp_sock); in BPF_CALL_1()