Home
last modified time | relevance | path

Searched refs:msk (Results 1 – 25 of 115) sorted by relevance

12345

/kernel/linux/linux-5.10/net/mptcp/
Dpm.c15 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr() argument
19 pr_debug("msk=%p, local_id=%d", msk, addr->id); in mptcp_pm_announce_addr()
21 msk->pm.local = *addr; in mptcp_pm_announce_addr()
22 WRITE_ONCE(msk->pm.add_addr_echo, echo); in mptcp_pm_announce_addr()
23 WRITE_ONCE(msk->pm.add_addr_signal, true); in mptcp_pm_announce_addr()
27 int mptcp_pm_remove_addr(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_addr() argument
29 pr_debug("msk=%p, local_id=%d", msk, local_id); in mptcp_pm_remove_addr()
31 msk->pm.rm_id = local_id; in mptcp_pm_remove_addr()
32 WRITE_ONCE(msk->pm.rm_addr_signal, true); in mptcp_pm_remove_addr()
36 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_subflow() argument
[all …]
Dprotocol.c29 struct mptcp_sock msk; member
48 static struct socket *__mptcp_nmpc_socket(const struct mptcp_sock *msk) in __mptcp_nmpc_socket() argument
50 if (!msk->subflow || READ_ONCE(msk->can_ack)) in __mptcp_nmpc_socket()
53 return msk->subflow; in __mptcp_nmpc_socket()
80 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback() argument
82 sock_owned_by_me((const struct sock *)msk); in __mptcp_tcp_fallback()
84 if (likely(!__mptcp_check_fallback(msk))) in __mptcp_tcp_fallback()
87 return msk->first; in __mptcp_tcp_fallback()
90 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create() argument
93 struct sock *sk = (struct sock *)msk; in __mptcp_socket_create()
[all …]
Dpm_netlink.c133 struct mptcp_sock *msk) in select_local_address() argument
138 spin_lock_bh(&msk->join_list_lock); in select_local_address()
146 if (entry->addr.family == ((struct sock *)msk)->sk_family && in select_local_address()
147 !lookup_subflow_by_saddr(&msk->conn_list, &entry->addr) && in select_local_address()
148 !lookup_subflow_by_saddr(&msk->join_list, &entry->addr)) { in select_local_address()
153 spin_unlock_bh(&msk->join_list_lock); in select_local_address()
182 static void check_work_pending(struct mptcp_sock *msk) in check_work_pending() argument
184 if (msk->pm.add_addr_signaled == msk->pm.add_addr_signal_max && in check_work_pending()
185 (msk->pm.local_addr_used == msk->pm.local_addr_max || in check_work_pending()
186 msk->pm.subflows == msk->pm.subflows_max)) in check_work_pending()
[all …]
Dtoken_test.c54 struct mptcp_sock *msk; in build_msk() local
56 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); in build_msk()
57 KUNIT_EXPECT_NOT_ERR_OR_NULL(test, msk); in build_msk()
58 refcount_set(&((struct sock *)msk)->sk_refcnt, 1); in build_msk()
59 sock_net_set((struct sock *)msk, &init_net); in build_msk()
60 return msk; in build_msk()
67 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
72 ctx->conn = (struct sock *)msk; in mptcp_token_test_msk_basic()
73 sk = (struct sock *)msk; in mptcp_token_test_msk_basic()
78 KUNIT_EXPECT_EQ(test, ctx->token, msk->token); in mptcp_token_test_msk_basic()
[all …]
Dprotocol.h245 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_tail() local
247 if (list_empty(&msk->rtx_queue)) in mptcp_rtx_tail()
250 return list_last_entry(&msk->rtx_queue, struct mptcp_data_frag, list); in mptcp_rtx_tail()
255 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head() local
257 return list_first_entry_or_null(&msk->rtx_queue, struct mptcp_data_frag, list); in mptcp_rtx_head()
274 struct mptcp_sock *msk; member
407 void mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk);
412 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit);
413 void mptcp_destroy_common(struct mptcp_sock *msk);
425 struct mptcp_sock *msk);
[all …]
Dmptcp_diag.c32 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one() local
39 msk = mptcp_token_get_sock(net, req->id.idiag_cookie[0]); in mptcp_diag_dump_one()
40 if (!msk) in mptcp_diag_dump_one()
44 sk = (struct sock *)msk; in mptcp_diag_dump_one()
77 struct mptcp_sock *msk; in mptcp_diag_dump() local
83 while ((msk = mptcp_token_iter_next(net, &cb->args[0], &cb->args[1])) != in mptcp_diag_dump()
85 struct inet_sock *inet = (struct inet_sock *)msk; in mptcp_diag_dump()
86 struct sock *sk = (struct sock *)msk; in mptcp_diag_dump()
116 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_diag_get_info() local
128 info->mptcpi_subflows = READ_ONCE(msk->pm.subflows); in mptcp_diag_get_info()
[all …]
Doptions.c489 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
497 snd_data_fin_enable = READ_ONCE(msk->snd_data_fin_enable); in mptcp_established_options_dss()
518 if (!READ_ONCE(msk->can_ack)) { in mptcp_established_options_dss()
523 if (READ_ONCE(msk->use_64bit_ack)) { in mptcp_established_options_dss()
525 opts->ext_copy.data_ack = READ_ONCE(msk->ack_seq); in mptcp_established_options_dss()
529 opts->ext_copy.data_ack32 = (uint32_t)READ_ONCE(msk->ack_seq); in mptcp_established_options_dss()
584 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
589 if (!mptcp_pm_should_add_signal(msk) || in mptcp_established_options_add_addr()
590 !(mptcp_pm_add_addr_signal(msk, remaining, &saddr, &echo))) in mptcp_established_options_add_addr()
603 opts->ahmac = add_addr_generate_hmac(msk->local_key, in mptcp_established_options_add_addr()
[all …]
Dtoken.c155 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
175 WRITE_ONCE(msk->token, subflow->token); in mptcp_token_new_connect()
176 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_new_connect()
191 struct mptcp_sock *msk) in mptcp_token_accept() argument
203 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); in mptcp_token_accept()
211 struct mptcp_sock *msk; in mptcp_token_exists() local
219 msk = mptcp_sk(sk); in mptcp_token_exists()
220 if (READ_ONCE(msk->token) == token) in mptcp_token_exists()
247 struct mptcp_sock *msk; in mptcp_token_get_sock() local
255 msk = mptcp_sk(sk); in mptcp_token_get_sock()
[all …]
Dsubflow.c39 if (subflow_req->msk) in subflow_req_destructor()
40 sock_put((struct sock *)subflow_req->msk); in subflow_req_destructor()
56 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow() argument
58 return mptcp_is_fully_established((void *)msk) && in mptcp_can_accept_new_subflow()
59 READ_ONCE(msk->pm.accept_subflow); in mptcp_can_accept_new_subflow()
68 struct mptcp_sock *msk; in subflow_token_join_request() local
71 msk = mptcp_token_get_sock(sock_net(req_to_sk(req)), subflow_req->token); in subflow_token_join_request()
72 if (!msk) { in subflow_token_join_request()
77 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
79 sock_put((struct sock *)msk); in subflow_token_join_request()
[all …]
Dsyncookies.c97 struct mptcp_sock *msk; in mptcp_token_join_cookie_init_state() local
111 msk = mptcp_token_get_sock(net, e->token); in mptcp_token_join_cookie_init_state()
112 if (!msk) { in mptcp_token_join_cookie_init_state()
122 subflow_req->msk = msk; in mptcp_token_join_cookie_init_state()
/kernel/linux/linux-5.10/tools/testing/selftests/powerpc/primitives/asm/
Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
45 FTR_ENTRY_LONG msk; \
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
63 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
65 #define END_FTR_SECTION(msk, val) \ argument
66 END_FTR_SECTION_NESTED(msk, val, 97)
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
69 END_FTR_SECTION_NESTED((msk), (msk), label)
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
[all …]
/kernel/linux/linux-5.10/arch/powerpc/include/asm/
Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
45 FTR_ENTRY_LONG msk; \
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
63 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup)
65 #define END_FTR_SECTION(msk, val) \ argument
66 END_FTR_SECTION_NESTED(msk, val, 97)
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
69 END_FTR_SECTION_NESTED((msk), (msk), label)
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
[all …]
/kernel/linux/linux-5.10/drivers/net/ethernet/netronome/nfp/flower/
Dmatch.c12 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci() argument
18 memset(msk, 0, sizeof(struct nfp_flower_meta_tci)); in nfp_flower_compile_meta_tci()
24 msk->nfp_flow_key_layer = key_type; in nfp_flower_compile_meta_tci()
25 msk->mask_id = ~0; in nfp_flower_compile_meta_tci()
44 msk->tci = cpu_to_be16(tmp_tci); in nfp_flower_compile_meta_tci()
79 struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, in nfp_flower_compile_mac() argument
83 memset(msk, 0, sizeof(struct nfp_flower_mac_mpls)); in nfp_flower_compile_mac()
92 ether_addr_copy(msk->mac_dst, &match.mask->dst[0]); in nfp_flower_compile_mac()
93 ether_addr_copy(msk->mac_src, &match.mask->src[0]); in nfp_flower_compile_mac()
124 msk->mpls_lse = cpu_to_be32(t_mpls); in nfp_flower_compile_mac()
[all …]
/kernel/linux/linux-5.10/kernel/irq/
Dmatrix.c130 const struct cpumask *msk) in matrix_find_best_cpu() argument
137 for_each_cpu(cpu, msk) { in matrix_find_best_cpu()
151 const struct cpumask *msk) in matrix_find_best_cpu_managed() argument
158 for_each_cpu(cpu, msk) { in matrix_find_best_cpu_managed()
210 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_reserve_managed() argument
214 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
231 for_each_cpu(cpu, msk) { in irq_matrix_reserve_managed()
251 void irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_remove_managed() argument
255 for_each_cpu(cpu, msk) { in irq_matrix_remove_managed()
285 int irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc_managed() argument
[all …]
Ddevres.c235 u32 msk; member
244 irq_remove_generic_chip(this->gc, this->msk, this->clr, this->set); in devm_irq_remove_generic_chip()
263 u32 msk, enum irq_gc_flags flags, in devm_irq_setup_generic_chip() argument
273 irq_setup_generic_chip(gc, msk, flags, clr, set); in devm_irq_setup_generic_chip()
276 dr->msk = msk; in devm_irq_setup_generic_chip()
Ddebugfs.c33 struct cpumask *msk; in irq_debug_show_masks() local
35 msk = irq_data_get_affinity_mask(data); in irq_debug_show_masks()
36 seq_printf(m, "affinity: %*pbl\n", cpumask_pr_args(msk)); in irq_debug_show_masks()
38 msk = irq_data_get_effective_affinity_mask(data); in irq_debug_show_masks()
39 seq_printf(m, "effectiv: %*pbl\n", cpumask_pr_args(msk)); in irq_debug_show_masks()
42 msk = desc->pending_mask; in irq_debug_show_masks()
43 seq_printf(m, "pending: %*pbl\n", cpumask_pr_args(msk)); in irq_debug_show_masks()
/kernel/linux/linux-5.10/drivers/clk/sprd/
Dpll.c54 u32 msk, u32 val) in sprd_pll_write() argument
66 regmap_write(common->regmap, offset, (reg & ~msk) | val); in sprd_pll_write()
173 cfg[index].msk = mask; in _sprd_pll_set_rate()
184 cfg[index].msk |= mask; in _sprd_pll_set_rate()
189 cfg[index].msk |= mask; in _sprd_pll_set_rate()
196 cfg[index].msk |= mask; in _sprd_pll_set_rate()
206 cfg[index].msk |= mask; in _sprd_pll_set_rate()
214 cfg[index].msk |= mask; in _sprd_pll_set_rate()
217 if (cfg[i].msk) { in _sprd_pll_set_rate()
218 sprd_pll_write(pll, i, cfg[i].msk, cfg[i].val); in _sprd_pll_set_rate()
[all …]
/kernel/linux/linux-5.10/drivers/net/ethernet/aquantia/atlantic/
Daq_hw_utils.c19 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, in aq_hw_write_reg_bit() argument
22 if (msk ^ ~0) { in aq_hw_write_reg_bit()
26 reg_new = (reg_old & (~msk)) | (val << shift); 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() argument
37 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift); in aq_hw_read_reg_bit()
/kernel/linux/linux-5.10/drivers/media/usb/pvrusb2/
Dpvrusb2-ctrl.c207 int msk; in pvr2_ctrl_get_valname() local
210 for (idx = 0, msk = 1; val; idx++, msk <<= 1) { in pvr2_ctrl_get_valname()
211 if (val & msk) { in pvr2_ctrl_get_valname()
291 static unsigned int gen_bitmask_string(int msk,int val,int msk_only, in gen_bitmask_string() argument
304 for (idx = 0, sm = 1; msk; idx++, sm <<= 1) { in gen_bitmask_string()
305 if (sm & msk) { in gen_bitmask_string()
306 msk &= ~sm; in gen_bitmask_string()
396 int msk; in parse_mtoken() local
398 for (idx = 0, msk = 1; valid_bits; idx++, msk <<= 1) { in parse_mtoken()
399 if (!(msk & valid_bits)) continue; in parse_mtoken()
[all …]
Dpvrusb2-debugifc.c14 unsigned long msk; member
252 u32 msk,val; in pvr2_debugifc_do1cmd() local
266 ret = debugifc_parse_unsigned_number(wptr,wlen,&msk); in pvr2_debugifc_do1cmd()
273 val = msk; in pvr2_debugifc_do1cmd()
274 msk = 0xffffffff; in pvr2_debugifc_do1cmd()
277 ret = pvr2_hdw_gpio_chg_dir(hdw,msk,val); in pvr2_debugifc_do1cmd()
279 ret = pvr2_hdw_gpio_chg_out(hdw,msk,val); in pvr2_debugifc_do1cmd()
/kernel/linux/linux-5.10/lib/vdso/
Dgettimeofday.c228 u32 msk; in __cvdso_clock_gettime_common() local
238 msk = 1U << clock; in __cvdso_clock_gettime_common()
239 if (likely(msk & VDSO_HRES)) in __cvdso_clock_gettime_common()
241 else if (msk & VDSO_COARSE) in __cvdso_clock_gettime_common()
243 else if (msk & VDSO_RAW) in __cvdso_clock_gettime_common()
357 u32 msk; in __cvdso_clock_getres_common() local
372 msk = 1U << clock; in __cvdso_clock_getres_common()
373 if (msk & (VDSO_HRES | VDSO_RAW)) { in __cvdso_clock_getres_common()
378 } else if (msk & VDSO_COARSE) { in __cvdso_clock_getres_common()
/kernel/liteos_a/testsuites/unittest/net/socket/smoke/
Dnet_socket_test_013.cpp151 unsigned int msk = 0; in GetNetmask() local
159 msk = (reinterpret_cast<struct sockaddr_in *>(&(ifr.ifr_addr)))->sin_addr.s_addr; in GetNetmask()
161 return msk; in GetNetmask()
176 unsigned int ip, msk, brdcast; in ClientsThread() local
195 msk = GetNetmask(fd, ifname[j]); in ClientsThread()
198 LogPrintln("[%d]<%d>%s: netmask %s", fd, thrNo, ifname[j], MyInetNtoa(msk)); in ClientsThread()
203 brdcast = ip | ~msk; in ClientsThread()
/kernel/linux/linux-5.10/arch/arm/plat-orion/
Dgpio.c458 u32 msk; in orion_gpio_dbg_show() local
461 msk = 1 << i; in orion_gpio_dbg_show()
462 is_out = !(io_conf & msk); in orion_gpio_dbg_show()
468 out & msk ? "hi" : "lo", in orion_gpio_dbg_show()
469 blink & msk ? "(blink )" : ""); in orion_gpio_dbg_show()
474 (data_in ^ in_pol) & msk ? "hi" : "lo", in orion_gpio_dbg_show()
475 in_pol & msk ? "lo" : "hi"); in orion_gpio_dbg_show()
476 if (!((edg_msk | lvl_msk) & msk)) { in orion_gpio_dbg_show()
480 if (edg_msk & msk) in orion_gpio_dbg_show()
482 if (lvl_msk & msk) in orion_gpio_dbg_show()
[all …]
/kernel/linux/linux-5.10/drivers/usb/mtu3/
Dmtu3_host.c43 u32 reg, msk, val; in ssusb_wakeup_ip_sleep_set() local
48 msk = WC1_IS_EN | WC1_IS_C(0xf) | WC1_IS_P; in ssusb_wakeup_ip_sleep_set()
53 msk = SSC_IP_SLEEP_EN | SSC_SPM_INT_EN; in ssusb_wakeup_ip_sleep_set()
54 val = enable ? msk : 0; in ssusb_wakeup_ip_sleep_set()
59 regmap_update_bits(ssusb->uwk, reg, msk, val); in ssusb_wakeup_ip_sleep_set()
/kernel/linux/linux-5.10/drivers/mtd/nand/raw/
Dnand_bbt.c86 uint8_t msk = (mark & BBT_ENTRY_MASK) << ((block & BBT_ENTRY_MASK) * 2); in bbt_mark_entry() local
87 chip->bbt[block >> BBT_ENTRY_SHIFT] |= msk; in bbt_mark_entry()
174 uint8_t msk = (uint8_t)((1 << bits) - 1); in read_bbt() local
213 uint8_t tmp = (dat >> j) & msk; in read_bbt()
214 if (tmp == msk) in read_bbt()
722 uint8_t msk[4]; in write_bbt() local
769 msk[2] = ~rcode; in write_bbt()
771 case 1: sft = 3; sftmsk = 0x07; msk[0] = 0x00; msk[1] = 0x01; in write_bbt()
772 msk[3] = 0x01; in write_bbt()
774 case 2: sft = 2; sftmsk = 0x06; msk[0] = 0x00; msk[1] = 0x01; in write_bbt()
[all …]

12345