| /linux/tools/testing/selftests/powerpc/primitives/asm/ |
| H A D | feature-fixups.h | 57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
81 #define END_FTR_SECTION(msk, val) \ argument
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO argument
88 END_FTR_SECTION_IFCLR(msk) global() argument
92 ALT_FTR_SECTION_END_NESTED(msk,val,label) global() argument
94 ALT_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
96 ALT_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
98 ALT_FTR_SECTION_END(msk,val) global() argument
100 ALT_FTR_SECTION_END_IFSET(msk) global() argument
102 ALT_FTR_SECTION_END_IFCLR(msk) global() argument
109 END_MMU_FTR_SECTION_NESTED(msk,val,label) global() argument
113 END_MMU_FTR_SECTION(msk,val) global() argument
116 END_MMU_FTR_SECTION_NESTED_IFSET(msk,label) global() argument
119 END_MMU_FTR_SECTION_NESTED_IFCLR(msk,label) global() argument
122 END_MMU_FTR_SECTION_IFSET(msk) global() argument
123 END_MMU_FTR_SECTION_IFCLR(msk) global() argument
128 ALT_MMU_FTR_SECTION_END_NESTED(msk,val,label) global() argument
130 ALT_MMU_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
132 ALT_MMU_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
134 ALT_MMU_FTR_SECTION_END(msk,val) global() argument
136 ALT_MMU_FTR_SECTION_END_IFSET(msk) global() argument
138 ALT_MMU_FTR_SECTION_END_IFCLR(msk) global() argument
145 END_FW_FTR_SECTION_NESTED(msk,val,label) global() argument
149 END_FW_FTR_SECTION(msk,val) global() argument
152 END_FW_FTR_SECTION_IFSET(msk) global() argument
153 END_FW_FTR_SECTION_IFCLR(msk) global() argument
158 ALT_FW_FTR_SECTION_END_NESTED(msk,val,label) global() argument
160 ALT_FW_FTR_SECTION_END_NESTED_IFSET(msk,label) global() argument
162 ALT_FW_FTR_SECTION_END_NESTED_IFCLR(msk,label) global() argument
164 ALT_FW_FTR_SECTION_END(msk,val) global() argument
166 ALT_FW_FTR_SECTION_END_IFSET(msk) global() argument
168 ALT_FW_FTR_SECTION_END_IFCLR(msk) global() argument
173 ASM_FTR_IF(section_if,section_else,msk,val) global() argument
180 ASM_FTR_IFSET(section_if,section_else,msk) global() argument
183 ASM_FTR_IFCLR(section_if,section_else,msk) global() argument
186 ASM_MMU_FTR_IF(section_if,section_else,msk,val) global() argument
193 ASM_MMU_FTR_IFSET(section_if,section_else,msk) global() argument
196 ASM_MMU_FTR_IFCLR(section_if,section_else,msk) global() argument
[all...] |
| /linux/arch/powerpc/include/asm/ |
| H A D | feature-fixups.h | 57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
81 #define END_FTR_SECTION(msk, val) \ argument
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
88 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
92 #define ALT_FTR_SECTION_END_NESTED(msk, val, label) \ argument
94 #define ALT_FTR_SECTION_END_NESTED_IFSET(msk, label) \ argument
96 #define ALT_FTR_SECTION_END_NESTED_IFCLR(msk, label) \ argument
98 #define ALT_FTR_SECTION_END(msk, val) \ argument
[all …]
|
| /linux/net/mptcp/ |
| H A D | pm.c | 107 static bool mptcp_pm_is_init_remote_addr(struct mptcp_sock *msk, in mptcp_pm_is_init_remote_addr() argument
135 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, in mptcp_lookup_anno_list_by_saddr() argument
150 bool mptcp_remove_anno_list_by_saddr(struct mptcp_sock *msk, in mptcp_remove_anno_list_by_saddr() argument
163 bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk) in mptcp_pm_sport_in_anno_list() argument
184 __mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) __mptcp_pm_send_ack() argument
205 mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) mptcp_pm_send_ack() argument
214 mptcp_pm_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_addr_send_ack() argument
241 mptcp_pm_mp_prio_send_ack(struct mptcp_sock * msk,struct mptcp_addr_info * addr,struct mptcp_addr_info * rem,u8 bkup) mptcp_pm_mp_prio_send_ack() argument
275 struct mptcp_sock *msk = entry->sock; mptcp_pm_add_timer() local
322 mptcp_pm_del_add_timer(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool check_id) mptcp_pm_del_add_timer() argument
346 mptcp_pm_alloc_anno_list(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_alloc_anno_list() argument
384 mptcp_pm_free_anno_list(struct mptcp_sock * msk) mptcp_pm_free_anno_list() argument
404 mptcp_pm_announce_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool echo) mptcp_pm_announce_addr() argument
432 mptcp_pm_remove_addr(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_remove_addr() argument
453 mptcp_pm_new_connection(struct mptcp_sock * msk,const struct sock * ssk,int server_side) mptcp_pm_new_connection() argument
463 mptcp_pm_allow_new_subflow(struct mptcp_sock * msk) mptcp_pm_allow_new_subflow() argument
502 mptcp_pm_schedule_work(struct mptcp_sock * msk,enum mptcp_pm_status new_status) mptcp_pm_schedule_work() argument
515 mptcp_pm_fully_established(struct mptcp_sock * msk,const struct sock * ssk) mptcp_pm_fully_established() argument
542 mptcp_pm_connection_closed(struct mptcp_sock * msk) mptcp_pm_connection_closed() argument
550 mptcp_pm_subflow_established(struct mptcp_sock * msk) mptcp_pm_subflow_established() argument
567 mptcp_pm_subflow_check_next(struct mptcp_sock * msk,const struct mptcp_subflow_context * subflow) mptcp_pm_subflow_check_next() argument
603 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_add_addr_received() local
634 mptcp_pm_add_addr_echoed(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_add_addr_echoed() argument
652 mptcp_pm_add_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_add_addr_send_ack() argument
660 mptcp_pm_rm_addr_or_subflow(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list,enum linux_mptcp_mib_field rm_type) mptcp_pm_rm_addr_or_subflow() argument
723 mptcp_pm_rm_addr_recv(struct mptcp_sock * msk) mptcp_pm_rm_addr_recv() argument
728 mptcp_pm_rm_subflow(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_subflow() argument
734 mptcp_pm_rm_addr_received(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_received() argument
757 struct mptcp_sock *msk; mptcp_pm_mp_prio_received() local
770 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_mp_fail_received() local
795 mptcp_pm_add_addr_signal(struct mptcp_sock * msk,const struct sk_buff * skb,unsigned int opt_size,unsigned int remaining,struct mptcp_addr_info * addr,bool * echo,bool * drop_other_suboptions) mptcp_pm_add_addr_signal() argument
842 mptcp_pm_rm_addr_signal(struct mptcp_sock * msk,unsigned int remaining,struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_signal() argument
872 mptcp_pm_get_local_id(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_get_local_id() argument
896 mptcp_pm_is_backup(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_is_backup() argument
908 mptcp_pm_subflows_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflows_chk_stale() argument
945 mptcp_pm_subflow_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflow_chk_stale() argument
964 mptcp_pm_worker(struct mptcp_sock * msk) mptcp_pm_worker() argument
989 mptcp_pm_destroy(struct mptcp_sock * msk) mptcp_pm_destroy() argument
997 mptcp_pm_data_reset(struct mptcp_sock * msk) mptcp_pm_data_reset() argument
1026 mptcp_pm_data_init(struct mptcp_sock * msk) mptcp_pm_data_init() argument
[all...] |
| H A D | sockopt.c | 20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback() argument
51 static void sockopt_seq_inc(struct mptcp_sock *msk) in sockopt_seq_inc() argument
58 mptcp_get_int_option(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen,int * val) mptcp_get_int_option() argument
70 mptcp_sol_socket_sync_intval(struct mptcp_sock * msk,int optname,int val) mptcp_sol_socket_sync_intval() argument
123 mptcp_sol_socket_intval(struct mptcp_sock * msk,int optname,int val) mptcp_sol_socket_intval() argument
138 mptcp_so_incoming_cpu(struct mptcp_sock * msk,int val) mptcp_so_incoming_cpu() argument
147 mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock * msk,int optname,int val) mptcp_setsockopt_sol_socket_tstamp() argument
172 mptcp_setsockopt_sol_socket_int(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_int() argument
205 mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_timestamping() argument
249 mptcp_setsockopt_sol_socket_linger(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket_linger() argument
290 mptcp_setsockopt_sol_socket(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_socket() argument
387 mptcp_setsockopt_v6(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v6() argument
582 mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock * msk,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_tcp_congestion() argument
625 __mptcp_setsockopt_set_val(struct mptcp_sock * msk,int max,int (* set_val)(struct sock *,int),int * msk_val,int val) __mptcp_setsockopt_set_val() argument
650 __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock * msk,int val) __mptcp_setsockopt_sol_tcp_cork() argument
670 __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock * msk,int val) __mptcp_setsockopt_sol_tcp_nodelay() argument
689 mptcp_setsockopt_sol_ip_set(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_ip_set() argument
735 mptcp_setsockopt_v4_set_tos(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v4_set_tos() argument
763 mptcp_setsockopt_v4(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_v4() argument
779 mptcp_setsockopt_first_sf_only(struct mptcp_sock * msk,int level,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_first_sf_only() argument
801 mptcp_setsockopt_all_sf(struct mptcp_sock * msk,int level,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_all_sf() argument
818 mptcp_setsockopt_sol_tcp(struct mptcp_sock * msk,int optname,sockptr_t optval,unsigned int optlen) mptcp_setsockopt_sol_tcp() argument
895 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_setsockopt() local
930 mptcp_getsockopt_first_sf_only(struct mptcp_sock * msk,int level,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_first_sf_only() argument
956 mptcp_diag_fill_info(struct mptcp_sock * msk,struct mptcp_info * info) mptcp_diag_fill_info() argument
1015 mptcp_getsockopt_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_info() argument
1099 mptcp_getsockopt_tcpinfo(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_tcpinfo() argument
1191 mptcp_getsockopt_subflow_addrs(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_subflow_addrs() argument
1289 mptcp_getsockopt_full_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_full_info() argument
1363 mptcp_put_int_option(struct mptcp_sock * msk,char __user * optval,int __user * optlen,int val) mptcp_put_int_option() argument
1392 mptcp_getsockopt_sol_tcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_tcp() argument
1438 mptcp_getsockopt_v4(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v4() argument
1463 mptcp_getsockopt_v6(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v6() argument
1483 mptcp_getsockopt_sol_mptcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_mptcp() argument
1503 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_getsockopt() local
1531 sync_socket_options(struct mptcp_sock * msk,struct sock * ssk) sync_socket_options() argument
1587 mptcp_sockopt_sync_locked(struct mptcp_sock * msk,struct sock * ssk) mptcp_sockopt_sync_locked() argument
[all...] |
| H A D | protocol.c | 35 struct mptcp_sock msk; global() member
56 mptcp_wnd_end(const struct mptcp_sock * msk) mptcp_wnd_end() argument
71 __mptcp_try_fallback(struct mptcp_sock * msk,int fb_mib) __mptcp_try_fallback() argument
91 __mptcp_socket_create(struct mptcp_sock * msk) __mptcp_socket_create() argument
121 __mptcp_nmpc_sk(struct mptcp_sock * msk) __mptcp_nmpc_sk() argument
172 mptcp_ooo_try_coalesce(struct mptcp_sock * msk,struct sk_buff * to,struct sk_buff * from) mptcp_ooo_try_coalesce() argument
185 mptcp_data_queue_ofo(struct mptcp_sock * msk,struct sk_buff * skb) mptcp_data_queue_ofo() argument
296 __mptcp_move_skb(struct mptcp_sock * msk,struct sock * ssk,struct sk_buff * skb,unsigned int offset,size_t copy_len) __mptcp_move_skb() argument
374 mptcp_shutdown_subflows(struct mptcp_sock * msk) mptcp_shutdown_subflows() argument
391 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_pending_data_fin_ack() local
400 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_data_fin_ack() local
424 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_pending_data_fin() local
497 mptcp_send_ack(struct mptcp_sock * msk) mptcp_send_ack() argument
528 mptcp_cleanup_rbuf(struct mptcp_sock * msk,int copied) mptcp_cleanup_rbuf() argument
549 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_data_fin() local
598 mptcp_dss_corruption(struct mptcp_sock * msk,struct sock * ssk) mptcp_dss_corruption() argument
606 __mptcp_move_skbs_from_subflow(struct mptcp_sock * msk,struct sock * ssk) __mptcp_move_skbs_from_subflow() argument
677 __mptcp_ofo_queue(struct mptcp_sock * msk) __mptcp_ofo_queue() argument
755 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_error_report() local
765 move_skbs_to_msk(struct mptcp_sock * msk,struct sock * ssk) move_skbs_to_msk() argument
797 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_data_ready() local
825 mptcp_subflow_joined(struct mptcp_sock * msk,struct sock * ssk) mptcp_subflow_joined() argument
832 __mptcp_finish_join(struct mptcp_sock * msk,struct sock * ssk) __mptcp_finish_join() argument
863 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_flush_join_list() local
926 mptcp_frag_can_collapse_to(const struct mptcp_sock * msk,const struct page_frag * pfrag,const struct mptcp_data_frag * df) mptcp_frag_can_collapse_to() argument
954 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_clean_una() local
1029 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_enter_memory_pressure() local
1058 mptcp_carve_data_frag(const struct mptcp_sock * msk,struct page_frag * pfrag,int orig_offset) mptcp_carve_data_frag() argument
1084 mptcp_check_allowed_size(const struct mptcp_sock * msk,struct sock * ssk,u64 data_seq,int avail_size) mptcp_check_allowed_size() argument
1169 mptcp_update_infinite_map(struct mptcp_sock * msk,struct sock * ssk,struct mptcp_ext * mpext) mptcp_update_infinite_map() argument
1196 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg_frag() local
1369 mptcp_subflow_get_send(struct mptcp_sock * msk) mptcp_subflow_get_send() argument
1451 mptcp_update_post_push(struct mptcp_sock * msk,struct mptcp_data_frag * dfrag,u32 sent) mptcp_update_post_push() argument
1490 struct mptcp_sock *msk = mptcp_sk(sk); __subflow_push_pending() local
1534 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_push_pending() local
1598 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_subflow_push_pending() local
1669 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg_fastopen() local
1742 const struct mptcp_sock *msk = mptcp_sk(sk); mptcp_send_limit() local
1761 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg() local
1896 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_recvmsg_mskq() local
1953 mptcp_rcv_space_adjust(struct mptcp_sock * msk,int copied) mptcp_rcv_space_adjust() argument
2050 __mptcp_first_ready_from(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow) __mptcp_first_ready_from() argument
2066 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_move_skbs() local
2112 const struct mptcp_sock *msk = mptcp_sk(sk); mptcp_inq_hint() local
2134 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_recvmsg() local
2252 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_retransmit_timer() local
2280 mptcp_subflow_get_retrans(struct mptcp_sock * msk) mptcp_subflow_get_retrans() argument
2319 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_retransmit_pending_data() local
2389 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close_ssk() local
2506 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close_subflow() local
2538 mptcp_check_fastclose(struct mptcp_sock * msk) mptcp_check_fastclose() argument
2590 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_retrans() local
2682 mptcp_reset_tout_timer(struct mptcp_sock * msk,unsigned long fail_tout) mptcp_reset_tout_timer() argument
2701 mptcp_mp_fail_no_response(struct mptcp_sock * msk) mptcp_mp_fail_no_response() argument
2720 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_do_fastclose() local
2730 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); mptcp_worker() local
2775 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_init_sock() local
2854 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_clear_xmit() local
2864 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_cancel_work() local
2958 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_send_data_fin() local
2982 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_wr_shutdown() local
2997 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_destroy_sock() local
3051 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close() local
3132 mptcp_copy_inaddrs(struct sock * msk,const struct sock * ssk) mptcp_copy_inaddrs() argument
3157 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_disconnect() local
3267 struct mptcp_sock *msk; mptcp_sk_clone_init() local
3339 mptcp_rcv_space_init(struct mptcp_sock * msk,const struct sock * ssk) mptcp_rcv_space_init() argument
3356 mptcp_destroy_common(struct mptcp_sock * msk,unsigned int flags) mptcp_destroy_common() argument
3379 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_destroy() local
3415 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_release_cb() local
3536 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_get_port() local
3548 struct mptcp_sock *msk; mptcp_finish_connect() local
3579 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_finish_join() local
3643 mptcp_ioctl_outq(const struct mptcp_sock * msk,u64 v) mptcp_ioctl_outq() argument
3674 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_ioctl() local
3708 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_connect() local
3817 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_bind() local
3844 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_listen() local
3885 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_stream_accept() local
3967 mptcp_check_writeable(struct mptcp_sock * msk) mptcp_check_writeable() argument
3986 struct mptcp_sock *msk; mptcp_poll() local
[all...] |
| H A D | pm_userspace.c | 15 void mptcp_userspace_pm_free_local_addr_list(struct mptcp_sock *msk) in mptcp_userspace_pm_free_local_addr_list() argument
31 mptcp_userspace_pm_lookup_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_lookup_addr() argument
43 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_append_new_local_addr() argument
98 mptcp_userspace_pm_delete_local_addr(struct mptcp_sock * msk,struct mptcp_pm_addr_entry * addr) mptcp_userspace_pm_delete_local_addr() argument
118 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock * msk,unsigned int id) mptcp_userspace_pm_lookup_addr_by_id() argument
129 mptcp_userspace_pm_get_local_id(struct mptcp_sock * msk,struct mptcp_pm_addr_entry * skc) mptcp_userspace_pm_get_local_id() argument
148 mptcp_userspace_pm_is_backup(struct mptcp_sock * msk,struct mptcp_addr_info * skc) mptcp_userspace_pm_is_backup() argument
164 struct mptcp_sock *msk; mptcp_userspace_pm_get_sock() local
190 struct mptcp_sock *msk; mptcp_pm_nl_announce_doit() local
246 mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock * msk) mptcp_userspace_pm_remove_id_zero_address() argument
277 mptcp_pm_remove_addr_entry(struct mptcp_sock * msk,struct mptcp_pm_addr_entry * entry) mptcp_pm_remove_addr_entry() argument
300 struct mptcp_sock *msk; mptcp_pm_nl_remove_doit() local
363 struct mptcp_sock *msk; mptcp_pm_nl_subflow_create_doit() local
430 mptcp_nl_find_ssk(struct mptcp_sock * msk,const struct mptcp_addr_info * local,const struct mptcp_addr_info * remote) mptcp_nl_find_ssk() argument
481 struct mptcp_sock *msk; mptcp_pm_nl_subflow_destroy_doit() local
561 struct mptcp_sock *msk; mptcp_userspace_pm_set_flags() local
629 struct mptcp_sock *msk; mptcp_userspace_pm_dump_addr() local
666 struct mptcp_sock *msk; mptcp_userspace_pm_get_addr() local
[all...] |
| H A D | pm_kernel.c | 39 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk() argument
49 u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_signal_max() argument
57 u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_accept_max() argument
65 u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk) in mptcp_pm_get_subflows_max() argument
73 u8 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock *msk) in mptcp_pm_get_local_addr_max() argument
104 select_local_address(const struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_local_address() argument
132 select_signal_address(struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_signal_address() argument
165 fill_remote_addresses_vec(struct mptcp_sock * msk,struct mptcp_addr_info * local,bool fullmesh,struct mptcp_addr_info * addrs) fill_remote_addresses_vec() argument
256 mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock * msk) mptcp_pm_create_subflow_or_signal_addr() argument
370 mptcp_pm_nl_fully_established(struct mptcp_sock * msk) mptcp_pm_nl_fully_established() argument
375 mptcp_pm_nl_subflow_established(struct mptcp_sock * msk) mptcp_pm_nl_subflow_established() argument
383 fill_local_addresses_vec(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * locals) fill_local_addresses_vec() argument
444 mptcp_pm_nl_add_addr_received(struct mptcp_sock * msk) mptcp_pm_nl_add_addr_received() argument
495 mptcp_pm_nl_rm_addr(struct mptcp_sock * msk,u8 rm_id) mptcp_pm_nl_rm_addr() argument
696 mptcp_pm_nl_get_local_id(struct mptcp_sock * msk,struct mptcp_pm_addr_entry * skc) mptcp_pm_nl_get_local_id() argument
725 mptcp_pm_nl_is_backup(struct mptcp_sock * msk,struct mptcp_addr_info * skc) mptcp_pm_nl_is_backup() argument
742 struct mptcp_sock *msk; mptcp_nl_add_subflow_or_signal_addr() local
848 mptcp_endp_get_local_id(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_endp_get_local_id() argument
854 mptcp_pm_remove_anno_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool force) mptcp_pm_remove_anno_addr() argument
876 __mark_subflow_endp_available(struct mptcp_sock * msk,u8 id) __mark_subflow_endp_available() argument
890 struct mptcp_sock *msk; mptcp_nl_remove_subflow_and_signal_addr() local
936 struct mptcp_sock *msk; mptcp_nl_remove_id_zero_address() local
1020 mptcp_pm_flush_addrs_and_subflows(struct mptcp_sock * msk,struct list_head * rm_list) mptcp_pm_flush_addrs_and_subflows() argument
1053 struct mptcp_sock *msk; mptcp_nl_flush_addrs_list() local
1234 mptcp_pm_nl_fullmesh(struct mptcp_sock * msk,struct mptcp_addr_info * addr) mptcp_pm_nl_fullmesh() argument
1255 struct mptcp_sock *msk; mptcp_pm_nl_set_flags_all() local
1327 mptcp_pm_nl_check_work_pending(struct mptcp_sock * msk) mptcp_pm_nl_check_work_pending() argument
1341 __mptcp_pm_kernel_worker(struct mptcp_sock * msk) __mptcp_pm_kernel_worker() argument
[all...] |
| H A D | sched.c | 19 static int mptcp_sched_default_get_send(struct mptcp_sock *msk) in mptcp_sched_default_get_send() argument
32 mptcp_sched_default_get_retrans(struct mptcp_sock * msk,struct mptcp_sched_data * data) mptcp_sched_default_get_retrans() argument
119 mptcp_init_sched(struct mptcp_sock * msk,struct mptcp_sched_ops * sched) mptcp_init_sched() argument
137 mptcp_release_sched(struct mptcp_sock * msk) mptcp_release_sched() argument
157 mptcp_sched_get_send(struct mptcp_sock * msk) mptcp_sched_get_send() argument
185 mptcp_sched_get_retrans(struct mptcp_sock * msk) mptcp_sched_get_retrans() argument
[all...] |
| H A D | options.c | 445 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp() local
558 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
650 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
714 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr() local
789 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose() local
834 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options() local
929 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established()
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()
1086 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 | pm_netlink.c | 290 bool mptcp_userspace_pm_active(const struct mptcp_sock *msk) in mptcp_userspace_pm_active() argument
345 const struct mptcp_sock *msk, in mptcp_event_put_token_and_ssk() argument
378 const struct mptcp_sock *msk, in mptcp_event_sub_established() argument
385 const struct mptcp_sock *msk, in mptcp_event_sub_closed() argument
407 const struct mptcp_sock *msk, in mptcp_event_created() argument
428 mptcp_event_addr_removed(const struct mptcp_sock * msk,uint8_t id) mptcp_event_addr_removed() argument
463 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_event_addr_announced() local
566 mptcp_event(enum mptcp_event_type type,const struct mptcp_sock * msk,const struct sock * ssk,gfp_t gfp) mptcp_event() argument
[all...] |
| H A D | subflow.c | 61 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow() argument
72 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac() local
88 struct mptcp_sock *msk; subflow_token_join_request() local
120 subflow_use_different_sport(struct mptcp_sock * msk,const struct sock * sk) subflow_use_different_sport() argument
452 subflow_use_different_dport(struct mptcp_sock * msk,const struct sock * sk) subflow_use_different_dport() argument
460 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_sync_state() local
479 subflow_set_remote_key(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,const struct mptcp_options_received * mp_opt) subflow_set_remote_key() argument
504 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_propagate_state() local
530 struct mptcp_sock *msk; subflow_finish_connect() local
632 struct mptcp_sock *msk = mptcp_sk(subflow->conn); subflow_chk_local_id() local
755 struct mptcp_sock *msk = subflow_req->msk; subflow_hmac_valid() local
796 __mptcp_subflow_fully_established(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,const struct mptcp_options_received * mp_opt) __mptcp_subflow_fully_established() argument
1107 get_mapping_status(struct sock * ssk,struct mptcp_sock * msk) get_mapping_status() argument
1286 subflow_sched_work_if_closed(struct mptcp_sock * msk,struct sock * ssk) subflow_sched_work_if_closed() argument
1310 mptcp_subflow_fail(struct mptcp_sock * msk,struct sock * ssk) mptcp_subflow_fail() argument
1351 struct mptcp_sock *msk; subflow_check_data_avail() local
1503 struct mptcp_sock *msk; subflow_data_ready() local
1608 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_subflow_connect() local
[all...] |
| H A D | token_test.c | 54 struct mptcp_sock *msk; in build_msk() local
75 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
97 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept() local
116 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed() local
|
| H A D | token.c | 154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
192 struct mptcp_sock *msk) in mptcp_token_accept()
214 struct mptcp_sock *msk; in mptcp_token_exists() local
250 struct mptcp_sock *msk; in mptcp_token_get_sock() local
375 void mptcp_token_destroy(struct mptcp_sock *msk) in mptcp_token_destroy()
|
| H A D | protocol.h | 374 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me() argument
415 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head() local
422 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next() local
432 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail() local
445 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_rtx_head() local
477 struct mptcp_sock *msk; global() member
775 mptcp_data_avail(const struct mptcp_sock * msk) mptcp_data_avail() argument
894 mptcp_data_fin_enabled(const struct mptcp_sock * msk) mptcp_data_fin_enabled() argument
911 const struct mptcp_sock *msk = mptcp_sk(sk); mptcp_stream_memory_free() local
1094 mptcp_pm_should_add_signal(struct mptcp_sock * msk) mptcp_pm_should_add_signal() argument
1100 mptcp_pm_should_add_signal_addr(struct mptcp_sock * msk) mptcp_pm_should_add_signal_addr() argument
1105 mptcp_pm_should_add_signal_echo(struct mptcp_sock * msk) mptcp_pm_should_add_signal_echo() argument
1110 mptcp_pm_should_rm_signal(struct mptcp_sock * msk) mptcp_pm_should_rm_signal() argument
1115 mptcp_pm_is_userspace(const struct mptcp_sock * msk) mptcp_pm_is_userspace() argument
1120 mptcp_pm_is_kernel(const struct mptcp_sock * msk) mptcp_pm_is_kernel() argument
1191 __mptcp_pm_close_subflow(struct mptcp_sock * msk) __mptcp_pm_close_subflow() argument
1197 mptcp_pm_close_subflow(struct mptcp_sock * msk) mptcp_pm_close_subflow() argument
1213 __mptcp_check_fallback(const struct mptcp_sock * msk) __mptcp_check_fallback() argument
1221 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_check_fallback() local
1226 __mptcp_has_initial_subflow(const struct mptcp_sock * msk) __mptcp_has_initial_subflow() argument
1241 struct mptcp_sock *msk; mptcp_try_fallback() local
1260 mptcp_early_fallback(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,int fb_mib) mptcp_early_fallback() argument
[all...] |
| H A D | mptcp_diag.c | 31 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one() local
202 struct sock *lsk = READ_ONCE(msk in mptcp_diag_get_info() local
158 struct mptcp_sock *msk; mptcp_diag_dump() local
[all...] |
| /linux/drivers/net/ethernet/netronome/nfp/flower/ |
| H A D | match.c | 12 struct nfp_flower_meta_tci *msk, u8 key_type) in nfp_flower_compile_meta()
24 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_tci()
53 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci()
96 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mac()
120 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mpls()
175 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mac_mpls()
189 struct nfp_flower_tp_ports *msk, in nfp_flower_compile_tport()
210 struct nfp_flower_ip_ext *msk, struct flow_rule *rule) in nfp_flower_compile_ip_ext()
287 struct nfp_flower_vlan *msk, bool outer_vlan) in nfp_flower_fill_vlan()
319 struct nfp_flower_vlan *msk, in nfp_flower_compile_vlan()
[all …]
|
| /linux/net/mctp/ |
| H A D | af_mctp.c | 55 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_bind() local
135 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_connect() local
194 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sendmsg() local
288 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_recvmsg() local
389 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_setsockopt() local
410 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_getsockopt() local
502 mctp_ioctl_alloctag(struct mctp_sock * msk,bool tagv2,unsigned long arg) mctp_ioctl_alloctag() argument
545 mctp_ioctl_droptag(struct mctp_sock * msk,bool tagv2,unsigned long arg) mctp_ioctl_droptag() argument
594 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); mctp_ioctl() local
653 struct mctp_sock *msk = container_of(timer, struct mctp_sock, mctp_sk_expire_keys() local
695 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sk_init() local
712 struct mctp_sock *msk; mctp_sk_hash() local
757 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); mctp_sk_unhash() local
[all...] |
| H A D | route.c | 57 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_lookup_bind_details() local
83 struct mctp_sock *msk; in mctp_lookup_bind() local
223 static struct mctp_sk_key *mctp_key_alloc(struct mctp_sock *msk, in mctp_key_alloc()
265 static int mctp_key_add(struct mctp_sk_key *key, struct mctp_sock *msk) in mctp_key_add()
435 struct mctp_sock *msk; in mctp_dst_input() local
703 struct mctp_sock *msk) in mctp_reserve_tag()
723 struct mctp_sk_key *mctp_alloc_local_tag(struct mctp_sock *msk, in mctp_alloc_local_tag()
807 static struct mctp_sk_key *mctp_lookup_prealloc_tag(struct mctp_sock *msk, in mctp_lookup_prealloc_tag()
1105 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_local_output() local
|
| /linux/kernel/irq/ |
| H A D | matrix.c | 136 const struct cpumask *msk) in matrix_find_best_cpu()
157 const struct cpumask *msk) in matrix_find_best_cpu_managed()
216 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_reserve_managed()
257 void irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_remove_managed()
292 int irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc_managed()
383 int irq_matrix_alloc(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc()
|
| /linux/tools/testing/selftests/bpf/progs/ |
| H A D | mptcp_sock.c | 32 struct mptcp_sock *msk; in _sockops() local
81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk, in BPF_PROG()
|
| /linux/drivers/net/ethernet/aquantia/atlantic/ |
| H A D | aq_hw_utils.c | 19 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit()
35 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) in aq_hw_read_reg_bit()
|
| /linux/drivers/media/usb/pvrusb2/ |
| H A D | pvrusb2-ctrl.c | 207 int msk; in pvr2_ctrl_get_valname() local
291 static unsigned int gen_bitmask_string(int msk,int val,int msk_only, in gen_bitmask_string()
380 int msk; in parse_mtoken() local
|
| /linux/lib/reed_solomon/ |
| H A D | encode_rs.c | 21 uint16_t msk = (uint16_t) rs->nn; variable
|
| /linux/drivers/isdn/mISDN/ |
| H A D | stack.c | 420 struct mISDN_sock *msk = container_of(ch, struct mISDN_sock, ch); in connect_layer1() local
564 struct mISDN_sock *msk = container_of(ch, struct mISDN_sock, ch); in delete_channel() local
|
| /linux/net/mctp/test/ |
| H A D | sock-test.c | 106 struct mctp_sock *msk; in mctp_test_sock_sendmsg_extaddr() local
155 struct mctp_sock *msk; in mctp_test_sock_recvmsg_extaddr() local
|