| /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 | 108 mptcp_pm_is_init_remote_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * remote) mptcp_pm_is_init_remote_addr() argument
136 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_lookup_anno_list_by_saddr() argument
151 mptcp_remove_anno_list_by_saddr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_remove_anno_list_by_saddr() argument
164 mptcp_pm_sport_in_anno_list(struct mptcp_sock * msk,const struct sock * sk) mptcp_pm_sport_in_anno_list() argument
185 __mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) __mptcp_pm_send_ack() argument
206 mptcp_pm_send_ack(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow,bool prio,bool backup) mptcp_pm_send_ack() argument
229 mptcp_pm_addr_send_ack_avoid_list(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_addr_send_ack_avoid_list() argument
268 mptcp_pm_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_addr_send_ack() argument
273 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
303 mptcp_adjust_add_addr_timeout(struct mptcp_sock * msk) mptcp_adjust_add_addr_timeout() argument
328 struct mptcp_sock *msk = entry->sock; mptcp_pm_add_timer() local
375 mptcp_pm_del_add_timer(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool check_id) mptcp_pm_del_add_timer() argument
404 mptcp_pm_alloc_anno_list(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_alloc_anno_list() argument
441 mptcp_pm_free_anno_list(struct mptcp_sock * msk) mptcp_pm_free_anno_list() argument
461 mptcp_pm_announce_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool echo) mptcp_pm_announce_addr() argument
489 mptcp_pm_remove_addr(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_remove_addr() argument
510 mptcp_pm_new_connection(struct mptcp_sock * msk,const struct sock * ssk,int server_side) mptcp_pm_new_connection() argument
520 mptcp_pm_allow_new_subflow(struct mptcp_sock * msk) mptcp_pm_allow_new_subflow() argument
560 mptcp_pm_schedule_work(struct mptcp_sock * msk,enum mptcp_pm_status new_status) mptcp_pm_schedule_work() argument
573 mptcp_pm_fully_established(struct mptcp_sock * msk,const struct sock * ssk) mptcp_pm_fully_established() argument
600 mptcp_pm_connection_closed(struct mptcp_sock * msk) mptcp_pm_connection_closed() argument
608 mptcp_pm_subflow_established(struct mptcp_sock * msk) mptcp_pm_subflow_established() argument
625 mptcp_pm_subflow_check_next(struct mptcp_sock * msk,const struct mptcp_subflow_context * subflow) mptcp_pm_subflow_check_next() argument
663 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_add_addr_received() local
697 mptcp_pm_add_addr_echoed(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_pm_add_addr_echoed() argument
715 mptcp_pm_add_addr_send_ack(struct mptcp_sock * msk) mptcp_pm_add_addr_send_ack() argument
723 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
786 mptcp_pm_rm_addr_recv(struct mptcp_sock * msk) mptcp_pm_rm_addr_recv() argument
791 mptcp_pm_rm_subflow(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_subflow() argument
797 mptcp_pm_rm_addr_received(struct mptcp_sock * msk,const struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_received() argument
820 struct mptcp_sock *msk; mptcp_pm_mp_prio_received() local
833 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_pm_mp_fail_received() local
858 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
905 mptcp_pm_rm_addr_signal(struct mptcp_sock * msk,unsigned int remaining,struct mptcp_rm_list * rm_list) mptcp_pm_rm_addr_signal() argument
935 mptcp_pm_get_local_id(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_get_local_id() argument
959 mptcp_pm_is_backup(struct mptcp_sock * msk,struct sock_common * skc) mptcp_pm_is_backup() argument
971 mptcp_pm_subflows_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflows_chk_stale() argument
1008 mptcp_pm_subflow_chk_stale(const struct mptcp_sock * msk,struct sock * ssk) mptcp_pm_subflow_chk_stale() argument
1027 mptcp_pm_worker(struct mptcp_sock * msk) mptcp_pm_worker() argument
1052 mptcp_pm_destroy(struct mptcp_sock * msk) mptcp_pm_destroy() argument
1060 mptcp_pm_data_reset(struct mptcp_sock * msk) mptcp_pm_data_reset() argument
1089 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
1017 mptcp_getsockopt_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_info() argument
1101 mptcp_getsockopt_tcpinfo(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_tcpinfo() argument
1193 mptcp_getsockopt_subflow_addrs(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_subflow_addrs() argument
1291 mptcp_getsockopt_full_info(struct mptcp_sock * msk,char __user * optval,int __user * optlen) mptcp_getsockopt_full_info() argument
1365 mptcp_put_int_option(struct mptcp_sock * msk,char __user * optval,int __user * optlen,int val) mptcp_put_int_option() argument
1394 mptcp_getsockopt_sol_tcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_tcp() argument
1440 mptcp_getsockopt_v4(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v4() argument
1465 mptcp_getsockopt_v6(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_v6() argument
1485 mptcp_getsockopt_sol_mptcp(struct mptcp_sock * msk,int optname,char __user * optval,int __user * optlen) mptcp_getsockopt_sol_mptcp() argument
1505 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_getsockopt() local
1533 sync_socket_options(struct mptcp_sock * msk,struct sock * ssk) sync_socket_options() argument
1589 mptcp_sockopt_sync_locked(struct mptcp_sock * msk,struct sock * ssk) mptcp_sockopt_sync_locked() argument
[all...] |
| H A D | protocol.c | 38 struct mptcp_sock msk; member
59 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) in mptcp_wnd_end() argument
76 bool __mptcp_try_fallback(struct mptcp_sock *msk, int fb_mib) in __mptcp_try_fallback() argument
103 __mptcp_socket_create(struct mptcp_sock * msk) __mptcp_socket_create() argument
133 __mptcp_nmpc_sk(struct mptcp_sock * msk) __mptcp_nmpc_sk() argument
195 mptcp_ooo_try_coalesce(struct mptcp_sock * msk,struct sk_buff * to,struct sk_buff * from) mptcp_ooo_try_coalesce() argument
210 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_rcvbuf_grow() local
243 mptcp_data_queue_ofo(struct mptcp_sock * msk,struct sk_buff * skb) mptcp_data_queue_ofo() argument
379 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_move_skb() local
427 mptcp_shutdown_subflows(struct mptcp_sock * msk) mptcp_shutdown_subflows() argument
444 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_pending_data_fin_ack() local
453 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_data_fin_ack() local
477 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_pending_data_fin() local
550 mptcp_send_ack(struct mptcp_sock * msk) mptcp_send_ack() argument
581 mptcp_cleanup_rbuf(struct mptcp_sock * msk,int copied) mptcp_cleanup_rbuf() argument
602 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_data_fin() local
648 mptcp_dss_corruption(struct mptcp_sock * msk,struct sock * ssk) mptcp_dss_corruption() argument
660 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_add_backlog() local
698 __mptcp_move_skbs_from_subflow(struct mptcp_sock * msk,struct sock * ssk,bool own_msk) __mptcp_move_skbs_from_subflow() argument
773 __mptcp_ofo_queue(struct mptcp_sock * msk) __mptcp_ofo_queue() argument
852 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_error_report() local
862 move_skbs_to_msk(struct mptcp_sock * msk,struct sock * ssk) move_skbs_to_msk() argument
882 mptcp_rcv_rtt_update(struct mptcp_sock * msk,struct mptcp_subflow_context * subflow) mptcp_rcv_rtt_update() argument
911 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_data_ready() local
932 mptcp_subflow_joined(struct mptcp_sock * msk,struct sock * ssk) mptcp_subflow_joined() argument
939 __mptcp_finish_join(struct mptcp_sock * msk,struct sock * ssk) __mptcp_finish_join() argument
964 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_flush_join_list() local
1031 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
1060 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_clean_una() local
1135 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_enter_memory_pressure() local
1165 mptcp_carve_data_frag(const struct mptcp_sock * msk,struct page_frag * pfrag,int orig_offset) mptcp_carve_data_frag() argument
1192 mptcp_check_allowed_size(const struct mptcp_sock * msk,struct sock * ssk,u64 data_seq,size_t avail_size) mptcp_check_allowed_size() argument
1278 mptcp_update_infinite_map(struct mptcp_sock * msk,struct sock * ssk,struct mptcp_ext * mpext) mptcp_update_infinite_map() argument
1305 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg_frag() local
1491 mptcp_subflow_get_send(struct mptcp_sock * msk) mptcp_subflow_get_send() argument
1573 mptcp_update_post_push(struct mptcp_sock * msk,struct mptcp_data_frag * dfrag,u32 sent) mptcp_update_post_push() argument
1612 struct mptcp_sock *msk = mptcp_sk(sk); __subflow_push_pending() local
1656 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_push_pending() local
1723 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_subflow_push_pending() local
1794 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg_fastopen() local
1867 const struct mptcp_sock *msk = mptcp_sk(sk); mptcp_send_limit() local
1884 mptcp_rps_record_subflows(const struct mptcp_sock * msk) mptcp_rps_record_subflows() argument
1900 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_sendmsg() local
2056 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_recvmsg_mskq() local
2119 mptcp_rcv_space_init(struct mptcp_sock * msk,const struct sock * ssk) mptcp_rcv_space_init() argument
2138 mptcp_rcv_space_adjust(struct mptcp_sock * msk,int copied) mptcp_rcv_space_adjust() argument
2195 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_move_skbs() local
2223 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_can_spool_backlog() local
2244 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_backlog_spooled() local
2270 const struct mptcp_sock *msk = mptcp_sk(sk); mptcp_inq_hint() local
2292 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_recvmsg() local
2404 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_retransmit_timer() local
2434 mptcp_subflow_get_retrans(struct mptcp_sock * msk) mptcp_subflow_get_retrans() argument
2473 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_retransmit_pending_data() local
2542 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close_ssk() local
2644 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_close_ssk() local
2683 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close_subflow() local
2716 mptcp_check_fastclose(struct mptcp_sock * msk) mptcp_check_fastclose() argument
2768 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_retrans() local
2873 mptcp_reset_tout_timer(struct mptcp_sock * msk,unsigned long fail_tout) mptcp_reset_tout_timer() argument
2892 mptcp_mp_fail_no_response(struct mptcp_sock * msk) mptcp_mp_fail_no_response() argument
2910 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_backlog_purge() local
2929 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_do_fastclose() local
2964 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); mptcp_worker() local
3013 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_init_sock() local
3096 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_clear_xmit() local
3106 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_cancel_work() local
3200 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_check_send_data_fin() local
3224 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_wr_shutdown() local
3239 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_destroy_sock() local
3293 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_close() local
3374 mptcp_copy_inaddrs(struct sock * msk,const struct sock * ssk) mptcp_copy_inaddrs() argument
3397 mptcp_destroy_common(struct mptcp_sock * msk) mptcp_destroy_common() argument
3421 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_disconnect() local
3537 struct mptcp_sock *msk; mptcp_sk_clone_init() local
3611 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_destroy() local
3643 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_release_cb() local
3769 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_get_port() local
3781 struct mptcp_sock *msk; mptcp_finish_connect() local
3830 struct mptcp_sock *msk = mptcp_sk(subflow->conn); mptcp_finish_join() local
3902 mptcp_ioctl_outq(const struct mptcp_sock * msk,u64 v) mptcp_ioctl_outq() argument
3933 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_ioctl() local
3968 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_connect() local
4077 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_bind() local
4104 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_listen() local
4145 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_graft_subflows() local
4208 struct mptcp_sock *msk = mptcp_sk(sock->sk); mptcp_stream_accept() local
4284 mptcp_check_writeable(struct mptcp_sock * msk) mptcp_check_writeable() argument
4303 struct mptcp_sock *msk; mptcp_poll() local
4350 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_recv_skb() local
4375 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_read_sock() local
[all...] |
| H A D | pm_kernel.c | 40 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk() argument
50 u8 mptcp_pm_get_endp_signal_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_signal_max() argument
58 u8 mptcp_pm_get_endp_subflow_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_subflow_max() argument
66 u8 mptcp_pm_get_endp_laminar_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_laminar_max() argument
74 u8 mptcp_pm_get_endp_fullmesh_max(const struct mptcp_sock *msk) in mptcp_pm_get_endp_fullmesh_max() argument
82 mptcp_pm_get_limit_add_addr_accepted(const struct mptcp_sock * msk) mptcp_pm_get_limit_add_addr_accepted() argument
90 mptcp_pm_get_limit_extra_subflows(const struct mptcp_sock * msk) mptcp_pm_get_limit_extra_subflows() argument
121 select_local_address(const struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_local_address() argument
149 select_signal_address(struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_signal_address() argument
180 fill_remote_addr(struct mptcp_sock * msk,struct mptcp_addr_info * local,struct mptcp_addr_info * addrs) fill_remote_addr() argument
202 fill_remote_addresses_fullmesh(struct mptcp_sock * msk,struct mptcp_addr_info * local,struct mptcp_addr_info * addrs) fill_remote_addresses_fullmesh() argument
250 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
289 mptcp_endp_get_local_id(struct mptcp_sock * msk,const struct mptcp_addr_info * addr) mptcp_endp_get_local_id() argument
296 mptcp_mpc_endpoint_setup(struct mptcp_sock * msk) mptcp_mpc_endpoint_setup() argument
329 mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock * msk) mptcp_pm_create_subflow_or_signal_addr() argument
433 mptcp_pm_nl_fully_established(struct mptcp_sock * msk) mptcp_pm_nl_fully_established() argument
438 mptcp_pm_nl_subflow_established(struct mptcp_sock * msk) mptcp_pm_nl_subflow_established() argument
444 fill_local_addresses_vec_fullmesh(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * locals,bool c_flag_case) fill_local_addresses_vec_fullmesh() argument
497 fill_local_laminar_endp(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * locals) fill_local_laminar_endp() argument
557 fill_local_addresses_vec_c_flag(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * locals) fill_local_addresses_vec_c_flag() argument
594 fill_local_address_any(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * local) fill_local_address_any() argument
619 fill_local_addresses_vec(struct mptcp_sock * msk,struct mptcp_addr_info * remote,struct mptcp_pm_local * locals) fill_local_addresses_vec() argument
643 mptcp_pm_nl_add_addr_received(struct mptcp_sock * msk) mptcp_pm_nl_add_addr_received() argument
692 mptcp_pm_nl_rm_addr(struct mptcp_sock * msk,u8 rm_id) mptcp_pm_nl_rm_addr() argument
904 mptcp_pm_nl_get_local_id(struct mptcp_sock * msk,struct mptcp_pm_addr_entry * skc) mptcp_pm_nl_get_local_id() argument
933 mptcp_pm_nl_is_backup(struct mptcp_sock * msk,struct mptcp_addr_info * skc) mptcp_pm_nl_is_backup() argument
950 struct mptcp_sock *msk; mptcp_nl_add_subflow_or_signal_addr() local
1042 mptcp_pm_remove_anno_addr(struct mptcp_sock * msk,const struct mptcp_addr_info * addr,bool force) mptcp_pm_remove_anno_addr() argument
1061 __mark_subflow_endp_available(struct mptcp_sock * msk,u8 id) __mark_subflow_endp_available() argument
1075 struct mptcp_sock *msk; mptcp_nl_remove_subflow_and_signal_addr() local
1119 struct mptcp_sock *msk; mptcp_nl_remove_id_zero_address() local
1211 mptcp_pm_flush_addrs_and_subflows(struct mptcp_sock * msk,struct list_head * rm_list) mptcp_pm_flush_addrs_and_subflows() argument
1244 struct mptcp_sock *msk; mptcp_nl_flush_addrs_list() local
1436 mptcp_pm_nl_fullmesh(struct mptcp_sock * msk,struct mptcp_addr_info * addr) mptcp_pm_nl_fullmesh() argument
1457 struct mptcp_sock *msk; mptcp_pm_nl_set_flags_all() local
1541 mptcp_pm_nl_check_work_pending(struct mptcp_sock * msk) mptcp_pm_nl_check_work_pending() argument
1555 __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 | pm_netlink.c | 291 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() local
572 void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk, in mptcp_event()
|
| 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 | 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
477 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
505 struct mptcp_sock *msk = mptcp_sk(sk); mptcp_propagate_state() local
531 struct mptcp_sock *msk; subflow_finish_connect() local
633 struct mptcp_sock *msk = mptcp_sk(subflow->conn); subflow_chk_local_id() local
756 struct mptcp_sock *msk = subflow_req->msk; subflow_hmac_valid() local
797 __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
1110 get_mapping_status(struct sock * ssk,struct mptcp_sock * msk) get_mapping_status() argument
1289 subflow_sched_work_if_closed(struct mptcp_sock * msk,struct sock * ssk) subflow_sched_work_if_closed() argument
1315 mptcp_subflow_fail(struct mptcp_sock * msk,struct sock * ssk) mptcp_subflow_fail() argument
1356 struct mptcp_sock *msk; subflow_check_data_avail() local
1511 struct mptcp_sock *msk; subflow_data_ready() local
1616 struct mptcp_sock *msk = mptcp_sk(sk); __mptcp_subflow_connect() local
[all...] |
| H A D | protocol.h | 392 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me()
434 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head() local
439 static inline void mptcp_init_rtt_est(struct mptcp_sock *msk) in mptcp_init_rtt_est()
449 static inline u32 mptcp_rtt_us_est(const struct mptcp_sock *msk) in mptcp_rtt_us_est()
462 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next() local
472 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail() local
485 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head() local
517 struct mptcp_sock *msk; member
858 static inline u64 mptcp_data_avail(const struct mptcp_sock *msk) in mptcp_data_avail()
980 static inline bool mptcp_data_fin_enabled(const struct mptcp_sock *msk) in mptcp_data_fin_enabled()
[all …]
|
| H A D | syncookies.c | 97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state() local
|
| /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()
438 struct mctp_sock *msk; in mctp_dst_input() local
709 struct mctp_sock *msk) in mctp_reserve_tag()
729 struct mctp_sk_key *mctp_alloc_local_tag(struct mctp_sock *msk, in mctp_alloc_local_tag()
813 static struct mctp_sk_key *mctp_lookup_prealloc_tag(struct mctp_sock *msk, in mctp_lookup_prealloc_tag()
1135 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_local_output() local
|
| /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 | 20 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit()
36 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
|
| H A D | pvrusb2-debug.h | 11 #define pvr2_trace(msk, fmt, arg...) do {if (msk & pvrusb2_debug) pr_info("pvrusb2: " fmt "\n", ##a… argument
|
| /linux/lib/reed_solomon/ |
| H A D | encode_rs.c | 21 uint16_t msk = (uint16_t) rs->nn; variable
|
| H A D | decode_rs.c | 26 uint16_t msk = (uint16_t) rs->nn; variable
|
| /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
|
| /linux/kernel/irq/ |
| H A D | devres.c | 282 u32 msk; member
310 u32 msk, enum irq_gc_flags flags, in devm_irq_setup_generic_chip()
|
| /linux/drivers/pinctrl/visconti/ |
| H A D | pinctrl-tmpv7700.c | 273 #define tmpv7700_GPIO_MUX(off, msk) \ argument
|
| /linux/drivers/perf/hisilicon/ |
| H A D | hisi_uncore_pa_pmu.c | 95 u32 msk = hisi_get_tgtid_msk(event); in hisi_pa_pmu_config_tgtid() local
117 u32 msk = hisi_get_srcid_msk(event); in hisi_pa_pmu_config_srcid() local
|