| /openbmc/linux/drivers/media/platform/sunxi/sun8i-di/ |
| H A D | sun8i-di.h | 43 #define DEINTERLACE_FIELD_CTRL_FIELD_CNT(v) ((v) & 0xff) argument
55 #define DEINTERLACE_IN_FMT_PS(v) ((v) & 3) argument
56 #define DEINTERLACE_IN_FMT_FMT(v) (((v) & 7) << 4) argument
57 #define DEINTERLACE_IN_FMT_MOD(v) (((v) & 7) << 8) argument
64 #define DEINTERLACE_OUT_FMT_FMT(v) ((v) & 0xf) argument
65 #define DEINTERLACE_OUT_FMT_PS(v) (((v) & 3) << 5) argument
90 #define DEINTERLACE_DIAG_INTP_TH0(v) ((v) & 0x7f) argument
92 #define DEINTERLACE_DIAG_INTP_TH1(v) (((v) & 0x7f) << 8) argument
106 #define DEINTERLACE_LUMA_TH_MIN_LUMA(v) ((v) & 0xff) argument
116 #define DEINTERLACE_SPAT_COMP_TH2(v) ((v) & 0xff) argument
[all …]
|
| /openbmc/linux/drivers/md/ |
| H A D | dm-verity-fec.c | 18 return v->fec && v->fec->dev; in verity_fec_is_enabled()
39 return offset + mod * (v->fec->rounds << v->data_dev_block_bits); in fec_interleave()
187 if (unlikely(verity_hash(v, verity_io_hash_req(v, io), in fec_is_erasure()
225 ileaved = fec_interleave(v, rsb * v->fec->rsn + i); in fec_read_bufs()
388 r = verity_hash(v, verity_io_hash_req(v, io), fio->output, in fec_decode_rsb()
438 block = block - v->hash_start + v->data_blocks; in verity_fec_decode()
457 rsb = offset - res * (v->fec->rounds << v->data_dev_block_bits); in verity_fec_decode()
566 v->fec = NULL; in verity_fec_dtr()
664 v->fec = f; in verity_fec_ctr_alloc()
700 hash_blocks = v->hash_blocks - v->hash_start; in verity_fec_ctr()
[all …]
|
| /openbmc/qemu/tests/unit/ |
| H A D | test-qobject-input-visitor.c | 71 Visitor *v; in visitor_input_test_init_full() local
78 return v; in visitor_input_test_init_full()
85 Visitor *v; in visitor_input_test_init() local
92 return v; in visitor_input_test_init()
115 Visitor *v; in test_visitor_in_int() local
133 Visitor *v; in test_visitor_in_uint() local
166 Visitor *v; in test_visitor_in_int_overflow() local
184 Visitor *v; in test_visitor_in_int_keyval() local
195 Visitor *v; in test_visitor_in_int_str_keyval() local
207 Visitor *v; in test_visitor_in_int_str_fail() local
[all …]
|
| /openbmc/linux/crypto/ |
| H A D | aegis128-neon-inner.c | 26 uint8x16_t v[5]; member
111 st.v[4] ^= aegis_aes_round(st.v[3]); in aegis128_update_neon()
112 st.v[3] ^= aegis_aes_round(st.v[2]); in aegis128_update_neon()
113 st.v[2] ^= aegis_aes_round(st.v[1]); in aegis128_update_neon()
114 st.v[1] ^= aegis_aes_round(st.v[0]); in aegis128_update_neon()
232 uint8x16_t s = st.v[1] ^ (st.v[2] & st.v[3]) ^ st.v[4]; in crypto_aegis128_encrypt_chunk_neon()
245 uint8x16_t s = st.v[1] ^ (st.v[2] & st.v[3]) ^ st.v[4]; in crypto_aegis128_encrypt_chunk_neon()
281 msg = vld1q_u8(src) ^ st.v[1] ^ (st.v[2] & st.v[3]) ^ st.v[4]; in crypto_aegis128_decrypt_chunk_neon()
291 uint8x16_t s = st.v[1] ^ (st.v[2] & st.v[3]) ^ st.v[4]; in crypto_aegis128_decrypt_chunk_neon()
334 v = st.v[0] ^ st.v[1] ^ st.v[2] ^ st.v[3] ^ st.v[4]; in crypto_aegis128_final_neon()
[all …]
|
| H A D | blake2b_generic.c | 60 G(r,0,v[ 0],v[ 4],v[ 8],v[12]); \
61 G(r,1,v[ 1],v[ 5],v[ 9],v[13]); \
62 G(r,2,v[ 2],v[ 6],v[10],v[14]); \
63 G(r,3,v[ 3],v[ 7],v[11],v[15]); \
64 G(r,4,v[ 0],v[ 5],v[10],v[15]); \
65 G(r,5,v[ 1],v[ 6],v[11],v[12]); \
66 G(r,6,v[ 2],v[ 7],v[ 8],v[13]); \
67 G(r,7,v[ 3],v[ 4],v[ 9],v[14]); \
74 u64 v[16]; in blake2b_compress_one_generic() local
81 v[i] = S->h[i]; in blake2b_compress_one_generic()
[all …]
|
| /openbmc/linux/arch/x86/kvm/ |
| H A D | irq.c | 61 if (!lapic_in_kernel(v)) in kvm_cpu_has_extint()
64 if (kvm_xen_has_interrupt(v)) in kvm_cpu_has_extint()
70 if (irqchip_split(v->kvm)) in kvm_cpu_has_extint()
84 if (kvm_cpu_has_extint(v)) in kvm_cpu_has_injectable_intr()
87 if (!is_guest_mode(v) && kvm_vcpu_apicv_active(v)) in kvm_cpu_has_injectable_intr()
100 if (kvm_cpu_has_extint(v)) in kvm_cpu_has_interrupt()
113 if (!kvm_cpu_has_extint(v)) { in kvm_cpu_get_extint()
118 if (!lapic_in_kernel(v)) in kvm_cpu_get_extint()
119 return v->arch.interrupt.nr; in kvm_cpu_get_extint()
121 if (kvm_xen_has_interrupt(v)) in kvm_cpu_get_extint()
[all …]
|
| /openbmc/linux/sound/soc/fsl/ |
| H A D | fsl_easrc.h | 115 #define EASRC_CC_BPS(v) (((v) << EASRC_CC_BPS_SHIFT) \ argument
127 #define EASRC_CC_CHEN(v) (((v) << EASRC_CC_CHEN_SHIFT) \ argument
193 #define EASRC_CIA_ITER(v) (((v) << EASRC_CIA_ITER_SHIFT) \ argument
296 #define EASRC_COC_BPS(v) (((v) << EASRC_COC_BPS_SHIFT) \ argument
319 #define EASRC_COA_ITER(v) (((v) << EASRC_COA_ITER_SHIFT) \ argument
342 #define EASRC_SFS_NSGI(v) (((v) << EASRC_SFS_NSGI_SHIFT) \ argument
351 #define EASRC_SFS_NSGO(v) (((v) << EASRC_SFS_NSGO_SHIFT) \ argument
357 #define EASRC_RRL_RS_RL(v) ((v) << EASRC_RRL_RS_RL_SHIFT) argument
396 #define EASRC_PCF_CD(v) ((v) << EASRC_PCF_CD_SHIFT) argument
463 #define EASRC_CSx_CSx(v) ((v) << EASRC_CSx_CSx_SHIFT) argument
[all …]
|
| /openbmc/u-boot/arch/arm/include/asm/arch-s32v234/ |
| H A D | siul.h | 78 #define SIUL2_MSCR_OBE(v) ((v) & 0x00200000) argument
81 #define SIUL2_MSCR_ODE(v) ((v) & 0x00100000) argument
84 #define SIUL2_MSCR_IBE(v) ((v) & 0x00010000) argument
87 #define SIUL2_MSCR_HYS(v) ((v) & 0x00400000) argument
90 #define SIUL2_MSCR_INV(v) ((v) & 0x00020000) argument
93 #define SIUL2_MSCR_PKE(v) ((v) & 0x00010000) argument
96 #define SIUL2_MSCR_SRE(v) ((v) & 0x0000C000) argument
102 #define SIUL2_MSCR_PUE(v) ((v) & 0x00002000) argument
105 #define SIUL2_MSCR_PUS(v) ((v) & 0x00001800) argument
111 #define SIUL2_MSCR_DSE(v) ((v) & 0x00000700) argument
[all …]
|
| /openbmc/linux/drivers/vhost/ |
| H A D | vdpa.c | 155 ops->kick_vq(v->vdpa, vq - v->vqs); in handle_vq_kick()
217 v->in_batch = 0; in vhost_vdpa_reset()
481 cb.private = v; in vhost_vdpa_set_config_call()
498 v->vdpa->config->set_config_cb(v->vdpa, &cb); in vhost_vdpa_set_config_call()
1159 if ((v->in_batch && v->batch_asid != asid) || !iotlb) { in vhost_vdpa_process_iotlb_msg()
1160 if (v->in_batch && v->batch_asid != asid) { in vhost_vdpa_process_iotlb_msg()
1448 kfree(v); in vhost_vdpa_release_dev()
1466 if (!v) in vhost_vdpa_probe()
1472 kfree(v); in vhost_vdpa_probe()
1500 r = cdev_device_add(&v->cdev, &v->dev); in vhost_vdpa_probe()
[all …]
|
| /openbmc/u-boot/include/asm-generic/ |
| H A D | atomic.h | 15 #define atomic_read(v) ((v)->counter) argument
16 #define atomic_set(v, i) ((v)->counter = (i)) argument
17 #define atomic64_read(v) atomic_read(v) argument
18 #define atomic64_set(v, i) atomic_set(v, i) argument
25 v->counter += i; in atomic_add()
34 v->counter -= i; in atomic_sub()
43 ++v->counter; in atomic_inc()
52 --v->counter; in atomic_dec()
62 val = v->counter; in atomic_dec_and_test()
98 v->counter += i; in atomic64_add()
[all …]
|
| /openbmc/qemu/qapi/ |
| H A D | qapi-dealloc-visitor.c | 115 static void qapi_dealloc_free(Visitor *v) in qapi_dealloc_free() argument
122 QapiDeallocVisitor *v; in qapi_dealloc_visitor_new() local
124 v = g_malloc0(sizeof(*v)); in qapi_dealloc_visitor_new()
126 v->visitor.type = VISITOR_DEALLOC; in qapi_dealloc_visitor_new()
131 v->visitor.next_list = qapi_dealloc_next_list; in qapi_dealloc_visitor_new()
132 v->visitor.end_list = qapi_dealloc_end_list; in qapi_dealloc_visitor_new()
135 v->visitor.type_bool = qapi_dealloc_type_bool; in qapi_dealloc_visitor_new()
136 v->visitor.type_str = qapi_dealloc_type_str; in qapi_dealloc_visitor_new()
139 v->visitor.type_null = qapi_dealloc_type_null; in qapi_dealloc_visitor_new()
140 v->visitor.free = qapi_dealloc_free; in qapi_dealloc_visitor_new()
[all …]
|
| /openbmc/linux/drivers/gpu/drm/amd/display/dc/dml/dcn32/ |
| H A D | display_mode_vba_32.c | 101 v->DISPCLK_calculated = v->WritebackDISPCLK; in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
138 &v->GlobalDPPCLK, v->DPPCLK); in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
141 v->DPPCLK_calculated[k] = v->DPPCLK[k]; in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
196 v->SwathWidthSingleDPPY, v->SwathWidthSingleDPPC, v->SwathWidthY, v->SwathWidthC, in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
206 v->ReadBandwidthSurfaceLuma[k] = v->SwathWidthSingleDPPY[k] * v->BytePerPixelY[k] in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
376 v->DSCDelay[k] = v->DSCDelay[j]; in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
515 v->VInitPreFillY, v->VInitPreFillC, in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
842 v->VStartup[k] = dml_min(v->VStartupLines, v->MaxVStartupLines[k]); in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
1192 v, in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
1193 v->PrefetchModePerState[v->VoltageLevel][v->maxMpcComb], in DISPCLKDPPCLKDCFCLKDeepSleepPrefetchParametersWatermarksAndPerformanceCalculation()
[all …]
|
| /openbmc/u-boot/drivers/usb/host/ |
| H A D | ehci-mxc.c | 66 unsigned int v; in mxc_set_usbcontrol() local
77 v |= MX25_OTG_PM_BIT; in mxc_set_usbcontrol()
80 v |= MX25_OTG_PP_BIT; in mxc_set_usbcontrol()
94 v |= MX25_H1_PM_BIT; in mxc_set_usbcontrol()
97 v |= MX25_H1_PP_BIT; in mxc_set_usbcontrol()
103 v |= MX25_H1_TLL_BIT; in mxc_set_usbcontrol()
133 v |= MX31_H1_PM_BIT; in mxc_set_usbcontrol()
136 v |= MX31_H1_DT_BIT; in mxc_set_usbcontrol()
144 v |= MX31_H2_PM_BIT; in mxc_set_usbcontrol()
147 v |= MX31_H2_DT_BIT; in mxc_set_usbcontrol()
[all …]
|
| /openbmc/linux/arch/alpha/kernel/ |
| H A D | termios.c | 7 struct termio v; in user_termio_to_kernel_termios() local
19 canon = v.c_lflag & ICANON; in user_termio_to_kernel_termios()
20 termios->c_cc[VINTR] = v.c_cc[_VINTR]; in user_termio_to_kernel_termios()
35 struct termio v; in kernel_termios_to_user_termio() local
38 memset(&v, 0, sizeof(struct termio)); in kernel_termios_to_user_termio()
39 v.c_iflag = termios->c_iflag; in kernel_termios_to_user_termio()
40 v.c_oflag = termios->c_oflag; in kernel_termios_to_user_termio()
41 v.c_cflag = termios->c_cflag; in kernel_termios_to_user_termio()
42 v.c_lflag = termios->c_lflag; in kernel_termios_to_user_termio()
43 v.c_line = termios->c_line; in kernel_termios_to_user_termio()
[all …]
|
| /openbmc/linux/include/linux/ |
| H A D | string_choices.h | 9 return v ? "enable" : "disable"; in str_enable_disable()
14 return v ? "enabled" : "disabled"; in str_enabled_disabled()
17 static inline const char *str_hi_lo(bool v) in str_hi_lo() argument
19 return v ? "hi" : "lo"; in str_hi_lo()
21 #define str_lo_hi(v) str_hi_lo(!(v)) argument
25 return v ? "high" : "low"; in str_high_low()
27 #define str_low_high(v) str_high_low(!(v)) argument
31 return v ? "read" : "write"; in str_read_write()
33 #define str_write_read(v) str_read_write(!(v)) argument
37 return v ? "on" : "off"; in str_on_off()
[all …]
|
| /openbmc/linux/drivers/pci/controller/ |
| H A D | pci-thunder-ecam.c | 21 v >>= shift; in set_val()
23 v &= 0xff; in set_val()
25 v &= 0xffff; in set_val()
26 *val = v; in set_val()
33 u32 v; in handle_ea_bar() local
47 v = readl(addr); in handle_ea_bar()
48 v &= ~0xf; in handle_ea_bar()
90 u32 v; in thunder_ecam_p2_config_read() local
107 v = readl(addr); in thunder_ecam_p2_config_read()
116 v |= node_bits; in thunder_ecam_p2_config_read()
[all …]
|
| /openbmc/linux/arch/x86/kernel/ |
| H A D | bootflag.c | 29 x ^= (v & 1); in parity()
30 v >>= 1; in parity()
42 if (!parity(v)) in sbf_write()
46 sbf_port, v); in sbf_write()
57 u8 v; in sbf_read() local
66 return v; in sbf_read()
73 if (!parity(v)) in sbf_value_valid()
81 u8 v; in sbf_init() local
86 v = sbf_read(); in sbf_init()
94 v &= ~SBF_DIAG; in sbf_init()
[all …]
|
| /openbmc/linux/sound/pci/emu10k1/ |
| H A D | emu10k1_patch.c | 40 if (sp->v.size == 0) { in snd_emu10k1_sample_new()
47 sp->v.end -= sp->v.start; in snd_emu10k1_sample_new()
48 sp->v.loopstart -= sp->v.start; in snd_emu10k1_sample_new()
49 sp->v.loopend -= sp->v.start; in snd_emu10k1_sample_new()
50 sp->v.start = 0; in snd_emu10k1_sample_new()
53 sampleend = sp->v.end; in snd_emu10k1_sample_new()
61 if (sp->v.loopstart >= sp->v.loopend) in snd_emu10k1_sample_new()
62 swap(sp->v.loopstart, sp->v.loopend); in snd_emu10k1_sample_new()
69 loopsize = sp->v.loopend - sp->v.loopstart; in snd_emu10k1_sample_new()
166 sp->v.loopstart = sp->v.end + BLANK_LOOP_START; in snd_emu10k1_sample_new()
[all …]
|
| /openbmc/qemu/include/qemu/ |
| H A D | bswap.h | 39 #define be_bswap(v, size) (v) argument
40 #define le_bswap(v, size) glue(__builtin_bswap, size)(v) argument
41 #define le_bswap24(v) bswap24(v) argument
42 #define be_bswaps(v, size) argument
46 #define le_bswap(v, size) (v) argument
47 #define le_bswap24(v) (v) argument
48 #define be_bswap(v, size) glue(__builtin_bswap, size)(v) argument
49 #define le_bswaps(v, size) argument
263 __builtin_memcpy(ptr, &v, sizeof(v)); in stw_he_p()
280 __builtin_memcpy(ptr, &v, sizeof(v)); in stl_he_p()
[all …]
|
| /openbmc/linux/arch/mips/include/asm/mach-bcm63xx/ |
| H A D | bcm63xx_io.h | 61 #define bcm_writeq(v, a) (*(volatile u64 *) BCM_REGS_VA((a)) = (v)) argument
69 #define bcm_rset_writeb(s, v, o) bcm_writeb((v), \ argument
71 #define bcm_rset_writew(s, v, o) bcm_writew((v), \ argument
73 #define bcm_rset_writel(s, v, o) bcm_writel((v), \ argument
80 #define bcm_perf_writel(v, o) bcm_rset_writel(RSET_PERF, (v), (o)) argument
84 #define bcm_wdt_writel(v, o) bcm_rset_writel(RSET_WDT, (v), (o)) argument
86 #define bcm_gpio_writel(v, o) bcm_rset_writel(RSET_GPIO, (v), (o)) argument
90 #define bcm_mpi_writel(v, o) bcm_rset_writel(RSET_MPI, (v), (o)) argument
94 #define bcm_pcie_writel(v, o) bcm_rset_writel(RSET_PCIE, (v), (o)) argument
98 #define bcm_memc_writel(v, o) bcm_rset_writel(RSET_MEMC, (v), (o)) argument
[all …]
|
| /openbmc/linux/drivers/media/platform/sunxi/sun6i-csi/ |
| H A D | sun6i_csi_reg.h | 18 #define SUN6I_CSI_EN_PTN_CYCLE(v) (((v) << 16) & GENMASK(23, 16)) argument
57 #define SUN6I_CSI_CAP_MASK(v) (((v) << 2) & GENMASK(5, 2)) argument
70 #define SUN6I_CSI_CH_CFG_PAD_VAL(v) (((v) << 24) & GENMASK(31, 24)) argument
71 #define SUN6I_CSI_CH_CFG_INPUT_FMT(v) (((v) << 20) & GENMASK(23, 20)) argument
161 #define SUN6I_CSI_CH_FLD1_VSIZE_VER_START(v) ((v) & GENMASK(12, 0)) argument
164 #define SUN6I_CSI_CH_HSIZE_LEN(v) (((v) << 16) & GENMASK(28, 16)) argument
165 #define SUN6I_CSI_CH_HSIZE_START(v) ((v) & GENMASK(12, 0)) argument
168 #define SUN6I_CSI_CH_VSIZE_LEN(v) (((v) << 16) & GENMASK(28, 16)) argument
169 #define SUN6I_CSI_CH_VSIZE_START(v) ((v) & GENMASK(12, 0)) argument
173 #define SUN6I_CSI_CH_BUF_LEN_LUMA_LINE(v) ((v) & GENMASK(13, 0)) argument
[all …]
|
| /openbmc/linux/sound/soc/qcom/ |
| H A D | lpass-cpu.c | 517 if (reg == LPAIF_WRDMACTL_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_writeable()
519 if (reg == LPAIF_WRDMABASE_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_writeable()
521 if (reg == LPAIF_WRDMABUFF_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_writeable()
523 if (reg == LPAIF_WRDMAPER_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_writeable()
563 if (reg == LPAIF_WRDMACTL_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_readable()
565 if (reg == LPAIF_WRDMABASE_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_readable()
567 if (reg == LPAIF_WRDMABUFF_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_readable()
569 if (reg == LPAIF_WRDMACURR_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_readable()
571 if (reg == LPAIF_WRDMAPER_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_readable()
596 if (reg == LPAIF_WRDMACURR_REG(v, i + v->wrdma_channel_start)) in lpass_cpu_regmap_volatile()
[all …]
|
| /openbmc/linux/drivers/base/regmap/ |
| H A D | regmap-fsi.c | 17 u32 v; in regmap_fsi32_reg_read() local
20 ret = fsi_slave_read(context, reg, &v, sizeof(v)); in regmap_fsi32_reg_read()
24 *val = v; in regmap_fsi32_reg_read()
32 return fsi_slave_write(context, reg, &v, sizeof(v)); in regmap_fsi32_reg_write()
42 __be32 v; in regmap_fsi32le_reg_read() local
45 ret = fsi_slave_read(context, reg, &v, sizeof(v)); in regmap_fsi32le_reg_read()
67 u16 v; in regmap_fsi16_reg_read() local
80 u16 v; in regmap_fsi16_reg_write() local
85 v = val; in regmap_fsi16_reg_write()
125 u8 v; in regmap_fsi8_reg_read() local
[all …]
|
| /openbmc/linux/arch/m68k/include/asm/ |
| H A D | atomic.h | 19 #define arch_atomic_read(v) READ_ONCE((v)->counter) argument
20 #define arch_atomic_set(v, i) WRITE_ONCE(((v)->counter), (i)) argument
92 t = v->counter; \
93 v->counter c_op i; \
157 : "=d" (c), "=m" (*v) in arch_atomic_dec_and_test_lt()
158 : "m" (*v)); in arch_atomic_dec_and_test_lt()
178 prev = arch_atomic_read(v); in arch_atomic_cmpxchg()
180 arch_atomic_set(v, new); in arch_atomic_cmpxchg()
192 prev = arch_atomic_read(v); in arch_atomic_xchg()
193 arch_atomic_set(v, new); in arch_atomic_xchg()
[all …]
|
| /openbmc/linux/arch/s390/include/asm/ |
| H A D | atomic.h | 20 return __atomic_read(v); in arch_atomic_read()
26 __atomic_set(v, i); in arch_atomic_set()
32 return __atomic_add_barrier(i, &v->counter) + i; in arch_atomic_add_return()
38 return __atomic_add_barrier(i, &v->counter); in arch_atomic_fetch_add()
44 __atomic_add(i, &v->counter); in arch_atomic_add()
55 __atomic_##op(i, &v->counter); \
75 #define arch_atomic_xchg(v, new) (arch_xchg(&((v)->counter), new)) in ATOMIC_OPS() argument
87 return __atomic64_read(v); in arch_atomic64_read()
93 __atomic64_set(v, i); in arch_atomic64_set()
111 __atomic64_add(i, (long *)&v->counter); in arch_atomic64_add()
[all …]
|