Home
last modified time | relevance | path

Searched refs:local_id (Results 1 – 25 of 37) sorted by relevance

12

/openbmc/linux/drivers/infiniband/core/
H A Dcm_trace.h146 __field(unsigned int, local_id)
154 __entry->local_id = be32_to_cpu(cm_id->local_id);
161 __entry->local_id, __entry->remote_id,
196 __field(u32, local_id)
204 __entry->local_id = be32_to_cpu(cm_id->local_id);
211 __entry->local_id, __entry->remote_id,
248 unsigned int local_id,
252 TP_ARGS(local_id, remote_id),
255 __field(unsigned int, local_id)
260 __entry->local_id = local_id;
[all …]
H A Dcm.c189 __be32 local_id; /* Established / timewait */ member
566 static u32 cm_local_id(__be32 local_id) in cm_local_id() argument
568 return (__force u32) (local_id ^ cm.random_id_operand); in cm_local_id()
571 static struct cm_id_private *cm_acquire_id(__be32 local_id, __be32 remote_id) in cm_acquire_id() argument
576 cm_id_priv = xa_load(&cm.local_id_table, cm_local_id(local_id)); in cm_acquire_id()
737 res = cm_acquire_id(timewait_info->work.local_id, in cm_find_remote_id()
836 cm_id_priv->id.local_id = (__force __be32)id ^ cm.random_id_operand; in cm_alloc_id_priv()
851 xa_store(&cm.local_id_table, cm_local_id(cm_id_priv->id.local_id), in cm_finalize_id()
959 static struct cm_timewait_info *cm_create_timewait_info(__be32 local_id) in cm_create_timewait_info() argument
967 timewait_info->work.local_id = local_id; in cm_create_timewait_info()
[all …]
/openbmc/linux/tools/lib/bpf/
H A Drelo_core.h71 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
73 int bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id,
75 int __bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
77 int bpf_core_types_match(const struct btf *local_btf, __u32 local_id, const struct btf *targ_btf,
H A Drelo_core.c146 int __bpf_core_types_are_compat(const struct btf *local_btf, __u32 local_id, in __bpf_core_types_are_compat() argument
153 local_type = btf_type_by_id(local_btf, local_id); in __bpf_core_types_are_compat()
163 local_type = skip_mods_and_typedefs(local_btf, local_id, &local_id); in __bpf_core_types_are_compat()
185 local_id = local_type->type; in __bpf_core_types_are_compat()
189 local_id = btf_array(local_type)->type; in __bpf_core_types_are_compat()
206 skip_mods_and_typedefs(local_btf, local_p->type, &local_id); in __bpf_core_types_are_compat()
208 err = __bpf_core_types_are_compat(local_btf, local_id, targ_btf, targ_id, in __bpf_core_types_are_compat()
215 skip_mods_and_typedefs(local_btf, local_type->type, &local_id); in __bpf_core_types_are_compat()
221 btf_kind_str(local_type), local_id, targ_id); in __bpf_core_types_are_compat()
413 __u32 local_id, in bpf_core_fields_are_compat() argument
[all …]
/openbmc/linux/drivers/firewire/
H A Dcore-card.c292 int root_id, new_root_id, irm_id, bm_id, local_id; in bm_work() local
327 local_id = card->local_node->node_id; in bm_work()
348 new_root_id = local_id; in bm_work()
355 new_root_id = local_id; in bm_work()
362 transaction_data[1] = cpu_to_be32(local_id); in bm_work()
380 bm_id == 0x3f ? local_id : 0xffc0 | bm_id; in bm_work()
385 if (local_id == irm_id) in bm_work()
410 new_root_id = local_id; in bm_work()
442 new_root_id = local_id; in bm_work()
453 new_root_id = local_id; in bm_work()
[all …]
/openbmc/linux/drivers/hwspinlock/
H A Dhwspinlock_internal.h67 int local_id = hwlock - &hwlock->bank->lock[0]; in hwlock_to_id() local
69 return hwlock->bank->base_id + local_id; in hwlock_to_id()
/openbmc/linux/net/mptcp/
H A Dsyncookies.c28 u8 local_id; member
67 entry->local_id = subflow_req->local_id; in mptcp_join_store_state()
H A Dsubflow.c89 int local_id; in subflow_token_join_request() local
97 local_id = mptcp_pm_get_local_id(msk, (struct sock_common *)req); in subflow_token_join_request()
98 if (local_id < 0) { in subflow_token_join_request()
102 subflow_req->local_id = local_id; in subflow_token_join_request()
596 static void subflow_set_local_id(struct mptcp_subflow_context *subflow, int local_id) in subflow_set_local_id() argument
598 WARN_ON_ONCE(local_id < 0 || local_id > 255); in subflow_set_local_id()
599 WRITE_ONCE(subflow->local_id, local_id); in subflow_set_local_id()
608 if (likely(subflow->local_id >= 0)) in subflow_chk_local_id()
1559 int local_id = loc->id; in __mptcp_subflow_connect() local
1581 if (local_id) in __mptcp_subflow_connect()
[all …]
H A Dprotocol.h425 u8 local_id; member
516 s16 local_id; /* if negative not initialized yet */
567 WRITE_ONCE(subflow->local_id, -1); in mptcp_subflow_ctx_reset()
1047 int local_id = READ_ONCE(subflow->local_id); in subflow_get_local_id()
1049 if (local_id < 0)
1051 return local_id;
1042 int local_id = READ_ONCE(subflow->local_id); subflow_get_local_id() local
/openbmc/linux/include/media/
H A Dv4l2-fwnode.h96 unsigned int local_id; member
H A Dmedia-entity.h466 static inline u32 media_gobj_gen_id(enum media_gobj_type type, u64 local_id) in media_gobj_gen_id() argument
471 id |= local_id & MEDIA_ID_MASK; in media_gobj_gen_id()
/openbmc/qemu/nbd/
H A Dclient.c724 uint32_t local_id; in nbd_receive_one_meta_context() local
750 if (reply.length <= sizeof(local_id) || in nbd_receive_one_meta_context()
759 if (nbd_read32(ioc, &local_id, "context id", errp) < 0) { in nbd_receive_one_meta_context()
763 reply.length -= sizeof(local_id); in nbd_receive_one_meta_context()
770 trace_nbd_opt_meta_reply(nbd_opt_lookup(opt), local_name, local_id); in nbd_receive_one_meta_context()
778 *id = local_id; in nbd_receive_one_meta_context()
/openbmc/linux/drivers/mailbox/
H A Dzynqmp-ipi-mailbox.c109 u32 local_id; member
126 a1 = pdata->local_id; in zynqmp_ipi_fw_call()
648 ret = of_property_read_u32(np, "xlnx,ipi-id", &pdata->local_id); in zynqmp_ipi_probe()
/openbmc/linux/drivers/staging/vt6656/
H A Dkey.c125 if (priv->local_id <= MAC_REVISION_A1) in vnt_set_keys()
H A Ddevice.h294 u8 local_id; member
/openbmc/linux/drivers/staging/vt6655/
H A Dkey.c83 bssid, (u32 *)key->key, priv->local_id); in vnt_set_keymode()
H A Dchannel.c113 if (priv->local_id > REV_ID_VT3253_B1) { in set_channel()
H A Ddpc.c103 if (priv->local_id > REV_ID_VT3253_A1) in vnt_rx_data()
H A Ddevice.h155 unsigned char local_id; member
H A Dmac.c775 unsigned char local_id) in MACvSetKeyEntry() argument
782 if (local_id <= 1) in MACvSetKeyEntry()
H A Dmac.h577 unsigned char local_id);
H A Dbaseband.c1996 unsigned char by_local_id = priv->local_id; in bb_vt3253_init()
H A Ddevice_main.c290 priv->local_id = ioread8(priv->port_offset + MAC_REG_LOCALID); in device_init_registers()
402 if (priv->local_id > REV_ID_VT3253_B1) { in device_init_registers()
468 if (priv->local_id <= REV_ID_VT3253_A1) in device_init_registers()
/openbmc/linux/include/rdma/
H A Dib_cm.h299 __be32 local_id; member
/openbmc/linux/tools/bpf/bpftool/
H A Dgen.c1999 btfgen_find_cands(const struct btf *local_btf, const struct btf *targ_btf, __u32 local_id) in btfgen_find_cands() argument
2009 local_cand.id = local_id; in btfgen_find_cands()
2011 local_type = btf__type_by_id(local_btf, local_id); in btfgen_find_cands()

12