Home
last modified time | relevance | path

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

/net/mptcp/
A Dprotocol.h273 struct mptcp_sock { struct
415 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head()
422 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next()
432 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail()
445 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head()
477 struct mptcp_sock *msk;
765 int mptcp_init_sched(struct mptcp_sock *msk,
911 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_stream_memory_free()
995 struct mptcp_sock *msk);
1183 void mptcp_pm_worker(struct mptcp_sock *msk);
[all …]
A Dpm.c20 struct mptcp_sock *sock;
205 void mptcp_pm_send_ack(struct mptcp_sock *msk, in mptcp_pm_send_ack()
214 void mptcp_pm_addr_send_ack(struct mptcp_sock *msk) in mptcp_pm_addr_send_ack()
275 struct mptcp_sock *msk = entry->sock; in mptcp_pm_add_timer()
317 mptcp_pm_del_add_timer(struct mptcp_sock *msk, in mptcp_pm_del_add_timer()
722 void mptcp_pm_rm_subflow(struct mptcp_sock *msk, in mptcp_pm_rm_subflow()
751 struct mptcp_sock *msk; in mptcp_pm_mp_prio_received()
958 void mptcp_pm_worker(struct mptcp_sock *msk) in mptcp_pm_worker()
983 void mptcp_pm_destroy(struct mptcp_sock *msk) in mptcp_pm_destroy()
991 void mptcp_pm_data_reset(struct mptcp_sock *msk) in mptcp_pm_data_reset()
[all …]
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()
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()
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()
763 static int mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_v4()
801 static int mptcp_setsockopt_all_sf(struct mptcp_sock *msk, int level, in mptcp_setsockopt_all_sf()
895 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_setsockopt()
1438 static int mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname, in mptcp_getsockopt_v4()
1463 static int mptcp_getsockopt_v6(struct mptcp_sock *msk, int optname, in mptcp_getsockopt_v6()
[all …]
A Dpm_userspace.c31 mptcp_userspace_pm_lookup_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_lookup_addr()
148 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, in mptcp_userspace_pm_is_backup()
164 struct mptcp_sock *msk; in mptcp_userspace_pm_get_sock()
190 struct mptcp_sock *msk; in mptcp_pm_nl_announce_doit()
277 void mptcp_pm_remove_addr_entry(struct mptcp_sock *msk, in mptcp_pm_remove_addr_entry()
300 struct mptcp_sock *msk; in mptcp_pm_nl_remove_doit()
363 struct mptcp_sock *msk; in mptcp_pm_nl_subflow_create_doit()
481 struct mptcp_sock *msk; in mptcp_pm_nl_subflow_destroy_doit()
561 struct mptcp_sock *msk; in mptcp_userspace_pm_set_flags()
629 struct mptcp_sock *msk; in mptcp_userspace_pm_dump_addr()
[all …]
A Dprotocol.c35 struct mptcp_sock msk;
377 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin_ack()
386 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin_ack()
409 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin()
534 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin()
739 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_error_report()
781 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_data_ready()
2714 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); in mptcp_worker()
3251 struct mptcp_sock *msk; in mptcp_sk_clone_init()
3532 struct mptcp_sock *msk; in mptcp_finish_connect()
[all …]
A Dtoken.c67 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 Dpm_kernel.c39 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk()
104 const struct mptcp_sock *msk, in select_local_address()
696 int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, in mptcp_pm_nl_get_local_id()
742 struct mptcp_sock *msk; in mptcp_nl_add_subflow_or_signal_addr()
848 static u8 mptcp_endp_get_local_id(struct mptcp_sock *msk, in mptcp_endp_get_local_id()
890 struct mptcp_sock *msk; in mptcp_nl_remove_subflow_and_signal_addr()
936 struct mptcp_sock *msk; in mptcp_nl_remove_id_zero_address()
1053 struct mptcp_sock *msk; in mptcp_nl_flush_addrs_list()
1235 static void mptcp_pm_nl_fullmesh(struct mptcp_sock *msk, in mptcp_pm_nl_fullmesh()
1256 struct mptcp_sock *msk; in mptcp_pm_nl_set_flags_all()
[all …]
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) in mptcp_sched_default_get_retrans()
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()
A Dpm_netlink.c290 bool mptcp_userspace_pm_active(const struct mptcp_sock *msk) in mptcp_userspace_pm_active()
345 const struct mptcp_sock *msk, in mptcp_event_put_token_and_ssk()
378 const struct mptcp_sock *msk, in mptcp_event_sub_established()
385 const struct mptcp_sock *msk, in mptcp_event_sub_closed()
407 const struct mptcp_sock *msk, in mptcp_event_created()
421 void mptcp_event_addr_removed(const struct mptcp_sock *msk, uint8_t id) in mptcp_event_addr_removed()
456 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_event_addr_announced()
559 void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk, in mptcp_event()
A Dsubflow.c72 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac()
88 struct mptcp_sock *msk; in subflow_token_join_request()
460 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_sync_state()
504 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_propagate_state()
530 struct mptcp_sock *msk; in subflow_finish_connect()
755 struct mptcp_sock *msk = subflow_req->msk; in subflow_hmac_valid()
817 struct mptcp_sock *owner; in subflow_syn_recv_sock()
1103 struct mptcp_sock *msk) in get_mapping_status()
1347 struct mptcp_sock *msk; in subflow_check_data_avail()
1499 struct mptcp_sock *msk; in subflow_data_ready()
[all …]
A Doptions.c445 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()
650 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr()
714 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr()
789 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose()
834 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options()
1038 static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) in __mptcp_snd_una_update()
1044 static void ack_update_msk(struct mptcp_sock *msk, in ack_update_msk()
1103 static bool add_addr_hmac_valid(struct mptcp_sock *msk, in add_addr_hmac_valid()
1125 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_incoming_options()
[all …]
A Dmptcp_diag.c31 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 Dbpf.c15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) in bpf_mptcp_sock_from_subflow()
A Dsyncookies.c97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state()
/net/core/
A Dfilter.c11924 BTF_TYPE_EMIT(struct mptcp_sock); in BPF_CALL_1()

Completed in 68 milliseconds