Home
last modified time | relevance | path

Searched defs:subflow (Results 1 – 18 of 18) sorted by relevance

/kernel/linux/linux-6.6/net/mptcp/
Dsubflow.c329 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_prep_synack() local
394 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid()
412 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_subflow_reset() local
439 struct mptcp_subflow_context *subflow; in __mptcp_sync_state() local
460 struct mptcp_subflow_context *subflow, in subflow_set_remote_key()
481 struct mptcp_subflow_context *subflow, in mptcp_propagate_state()
507 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_finish_connect() local
598 static void subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) in subflow_set_local_id()
606 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_chk_local_id() local
650 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v4_conn_request() local
[all …]
Doptions.c404 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_syn_options() local
445 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp() local
525 static void mptcp_write_data_fin(struct mptcp_subflow_context *subflow, in mptcp_write_data_fin()
558 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_dss() local
650 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_add_addr() local
714 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rm_addr() local
744 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp_prio() local
770 const struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rst() local
789 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_fastclose() local
812 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp_fail() local
[all …]
Dprotocol.c70 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
345 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skb() local
485 static long mptcp_timeout_from_subflow(const struct mptcp_subflow_context *subflow) in mptcp_timeout_from_subflow()
495 struct mptcp_subflow_context *subflow; in mptcp_set_timeout() local
526 struct mptcp_subflow_context *subflow; in mptcp_send_ack() local
558 struct mptcp_subflow_context *subflow; in mptcp_cleanup_rbuf() local
639 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skbs_from_subflow() local
811 struct mptcp_subflow_context *subflow; in __mptcp_error_report() local
848 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_data_ready() local
912 struct mptcp_subflow_context *tmp, *subflow; in __mptcp_flush_join_list() local
[all …]
Dsockopt.c72 struct mptcp_subflow_context *subflow; in mptcp_sol_socket_sync_intval() local
150 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_tstamp() local
210 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_timestamping() local
252 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_socket_linger() local
584 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_sol_tcp_congestion() local
628 struct mptcp_subflow_context *subflow; in __mptcp_setsockopt_set_val() local
651 struct mptcp_subflow_context *subflow; in __mptcp_setsockopt_sol_tcp_cork() local
671 struct mptcp_subflow_context *subflow; in __mptcp_setsockopt_sol_tcp_nodelay() local
729 struct mptcp_subflow_context *subflow; in mptcp_setsockopt_v4_set_tos() local
1054 struct mptcp_subflow_context *subflow; in mptcp_getsockopt_tcpinfo() local
[all …]
Dsched.c118 void mptcp_subflow_set_scheduled(struct mptcp_subflow_context *subflow, in mptcp_subflow_set_scheduled()
126 struct mptcp_subflow_context *subflow; in mptcp_sched_get_send() local
155 struct mptcp_subflow_context *subflow; in mptcp_sched_get_retrans() local
Dfastopen.c9 void mptcp_fastopen_subflow_synack_set_params(struct mptcp_subflow_context *subflow, in mptcp_fastopen_subflow_synack_set_params()
62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_fastopen_gen_msk_ackseq()
Dpm.c178 const struct mptcp_subflow_context *subflow) in mptcp_pm_subflow_check_next()
212 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_add_addr_received() local
288 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_mp_prio_received() local
302 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_pm_mp_fail_received() local
462 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_subflow_chk_stale() local
Dprotocol.h565 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock()
571 mptcp_subflow_ctx_reset(struct mptcp_subflow_context *subflow) in mptcp_subflow_ctx_reset()
579 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_map_offset()
587 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_mapped_dsn()
594 static inline void mptcp_subflow_delegate(struct mptcp_subflow_context *subflow, int action) in mptcp_subflow_delegate()
718 static inline bool __mptcp_subflow_active(struct mptcp_subflow_context *subflow) in __mptcp_subflow_active()
826 struct mptcp_subflow_context *subflow; in __mptcp_sync_sndbuf() local
850 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_propagate_sndbuf() local
863 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_propagate_sndbuf() local
1053 static inline u8 subflow_get_local_id(const struct mptcp_subflow_context *subflow) in subflow_get_local_id()
[all …]
Dpm_netlink.c118 struct mptcp_subflow_context *subflow; in lookup_subflow_by_saddr() local
136 struct mptcp_subflow_context *subflow; in lookup_subflow_by_daddr() local
426 struct mptcp_subflow_context *subflow; in fill_remote_addresses_vec() local
484 static void __mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in __mptcp_pm_send_ack()
503 static void mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, in mptcp_pm_send_ack()
554 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(msk->first); in mptcp_pm_create_subflow_or_signal_addr() local
786 struct mptcp_subflow_context *subflow; in mptcp_pm_nl_addr_send_ack() local
808 struct mptcp_subflow_context *subflow; in mptcp_pm_nl_mp_prio_send_ack() local
837 struct mptcp_subflow_context *subflow, *tmp; in mptcp_pm_nl_rm_addr_or_subflow() local
1235 struct mptcp_subflow_context *iter, *subflow = mptcp_subflow_ctx(ssk); in mptcp_pm_nl_subflow_chk_stale() local
[all …]
Dpm_userspace.c256 struct mptcp_subflow_context *subflow; in mptcp_userspace_pm_remove_id_zero_address() local
433 struct mptcp_subflow_context *subflow; in mptcp_nl_find_ssk() local
545 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_nl_cmd_sf_destroy() local
Dtoken.c153 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_token_new_connect() local
/kernel/linux/linux-5.10/net/mptcp/
Dsubflow.c255 static bool subflow_thmac_valid(struct mptcp_subflow_context *subflow) in subflow_thmac_valid()
275 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_subflow_reset() local
287 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_finish_connect() local
365 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v4_conn_request() local
395 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_v6_conn_request() local
514 void mptcp_subflow_fully_established(struct mptcp_subflow_context *subflow, in mptcp_subflow_fully_established()
683 static void dbg_bad_map(struct mptcp_subflow_context *subflow, u32 ssn) in dbg_bad_map()
691 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in skb_is_fully_mapped() local
704 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in validate_mapping() local
726 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in get_mapping_status() local
[all …]
Doptions.c336 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_syn_options() local
398 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_mp() local
456 static void mptcp_write_data_fin(struct mptcp_subflow_context *subflow, in mptcp_write_data_fin()
489 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_dss() local
584 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_add_addr() local
632 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_established_options_rm_addr() local
725 struct mptcp_subflow_context *subflow, in check_fully_established()
887 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_incoming_options() local
Dprotocol.c92 struct mptcp_subflow_context *subflow; in __mptcp_socket_create() local
268 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skb() local
415 struct mptcp_subflow_context *subflow; in mptcp_check_data_fin() local
464 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in __mptcp_move_skbs_from_subflow() local
625 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk); in mptcp_data_ready() local
708 struct mptcp_subflow_context *subflow; in mptcp_check_for_eof() local
739 struct mptcp_subflow_context *subflow; in mptcp_subflow_recv_lookup() local
794 struct mptcp_subflow_context *subflow; in mptcp_is_writeable() local
1049 struct mptcp_subflow_context *subflow; in mptcp_nospace() local
1064 static bool mptcp_subflow_active(struct mptcp_subflow_context *subflow) in mptcp_subflow_active()
[all …]
Dprotocol.h224 struct socket *subflow; /* outgoing connect/listener/!mp_capable */ member
345 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow) in mptcp_subflow_tcp_sock()
351 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_map_offset()
359 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow) in mptcp_subflow_get_mapped_dsn()
513 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_check_fallback() local
530 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_do_fallback() local
540 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in subflow_simultaneous_connect() local
Dpm_netlink.c116 struct mptcp_subflow_context *subflow; in lookup_subflow_by_saddr() local
402 struct mptcp_subflow_context *subflow, *tmp; in mptcp_pm_nl_rm_addr_received() local
438 struct mptcp_subflow_context *subflow, *tmp; in mptcp_pm_nl_rm_subflow_received() local
Dpm.c121 struct mptcp_subflow_context *subflow) in mptcp_pm_subflow_established()
Dtoken.c154 struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk); in mptcp_token_new_connect() local