arch/alpha/include/asm/io.h

134

#define REMAP1(TYPE, NAME, QUAL) \

arch/alpha/include/asm/io.h

135

static inline TYPE generic_##NAME(QUAL void __iomem *addr) \

arch/alpha/include/asm/io.h

140

#define REMAP2(TYPE, NAME, QUAL) \

arch/alpha/include/asm/io.h

141

static inline void generic_##NAME(TYPE b, QUAL void __iomem *addr) \

arch/alpha/include/asm/pal.h

18

#define __CALL_PAL_R0(NAME, TYPE) \

arch/alpha/include/asm/pal.h

19

extern inline TYPE NAME(void) \

arch/alpha/include/asm/pal.h

21

register TYPE __r0 __asm__("$0"); \

arch/arm64/kernel/cpufeature.c

192

#define __ARM64_FTR_BITS(SIGNED, VISIBLE, STRICT, TYPE, SHIFT, WIDTH, SAFE_VAL) \

arch/arm64/kernel/cpufeature.c

197

.type = TYPE, \

arch/arm64/kernel/cpufeature.c

204

#define ARM64_FTR_BITS(VISIBLE, STRICT, TYPE, SHIFT, WIDTH, SAFE_VAL) \

arch/arm64/kernel/cpufeature.c

205

__ARM64_FTR_BITS(FTR_UNSIGNED, VISIBLE, STRICT, TYPE, SHIFT, WIDTH, SAFE_VAL)

arch/arm64/kernel/cpufeature.c

208

#define S_ARM64_FTR_BITS(VISIBLE, STRICT, TYPE, SHIFT, WIDTH, SAFE_VAL) \

arch/arm64/kernel/cpufeature.c

209

__ARM64_FTR_BITS(FTR_SIGNED, VISIBLE, STRICT, TYPE, SHIFT, WIDTH, SAFE_VAL)

arch/loongarch/include/uapi/asm/kvm.h

92

#define LOONGARCH_REG_64(TYPE, REG) (TYPE | KVM_REG_SIZE_U64 | (REG << LOONGARCH_REG_SHIFT))

arch/mips/include/asm/octeon/cvmx.h

212

#define CVMX_BUILD_WRITE64(TYPE, ST) \

arch/mips/include/asm/octeon/cvmx.h

213

static inline void cvmx_write64_##TYPE(uint64_t addr, TYPE##_t val) \

arch/mips/include/asm/octeon/cvmx.h

215

*CASTPTR(volatile TYPE##_t, addr) = val; \

arch/mips/include/asm/octeon/cvmx.h

226

#define CVMX_BUILD_READ64(TYPE, LT) \

arch/mips/include/asm/octeon/cvmx.h

227

static inline TYPE##_t cvmx_read64_##TYPE(uint64_t addr) \

arch/mips/include/asm/octeon/cvmx.h

229

return *CASTPTR(volatile TYPE##_t, addr); \

arch/riscv/include/asm/vector.h

25

#define __riscv_v_vstate_or(_val, TYPE) ({ \

arch/riscv/include/asm/vector.h

28

_res = (_res & ~SR_VS_THEAD) | SR_VS_##TYPE##_THEAD; \

arch/riscv/include/asm/vector.h

30

_res = (_res & ~SR_VS) | SR_VS_##TYPE; \

arch/riscv/include/asm/vector.h

34

#define __riscv_v_vstate_check(_val, TYPE) ({ \

arch/riscv/include/asm/vector.h

37

_res = ((_val) & SR_VS_THEAD) == SR_VS_##TYPE##_THEAD; \

arch/riscv/include/asm/vector.h

39

_res = ((_val) & SR_VS) == SR_VS_##TYPE; \

arch/sparc/include/asm/asm.h

10

#define BRANCH32(TYPE, PREDICT, DEST) \

arch/sparc/include/asm/asm.h

11

TYPE,PREDICT %icc, DEST

arch/sparc/include/asm/asm.h

12

#define BRANCH32_ANNUL(TYPE, PREDICT, DEST) \

arch/sparc/include/asm/asm.h

13

TYPE,a,PREDICT %icc, DEST

arch/sparc/include/asm/asm.h

23

#define BRANCH32(TYPE, PREDICT, DEST) \

arch/sparc/include/asm/asm.h

24

TYPE DEST

arch/sparc/include/asm/asm.h

25

#define BRANCH32_ANNUL(TYPE, PREDICT, DEST) \

arch/sparc/include/asm/asm.h

26

TYPE,a DEST

arch/sparc/include/asm/vio.h

471

#define viodbg(TYPE, f, a...) \

arch/sparc/include/asm/vio.h

472

do { if (vio->debug & VIO_DEBUG_##TYPE) \

arch/sparc/kernel/ldc.c

176

#define ldcdbg(TYPE, f, a...) \

arch/sparc/kernel/ldc.c

177

do { if (lp->cfg.debug & LDC_DEBUG_##TYPE) \

arch/sparc/math-emu/math_32.c

298

case FSQRTQ: TYPE(3,3,1,3,1,0,0); break;

arch/sparc/math-emu/math_32.c

302

case FDIVQ: TYPE(3,3,1,3,1,3,1); break;

arch/sparc/math-emu/math_32.c

303

case FDMULQ: TYPE(3,3,1,2,1,2,1); break;

arch/sparc/math-emu/math_32.c

304

case FQTOS: TYPE(3,1,1,3,1,0,0); break;

arch/sparc/math-emu/math_32.c

305

case FQTOD: TYPE(3,2,1,3,1,0,0); break;

arch/sparc/math-emu/math_32.c

306

case FITOQ: TYPE(3,3,1,1,0,0,0); break;

arch/sparc/math-emu/math_32.c

307

case FSTOQ: TYPE(3,3,1,1,1,0,0); break;

arch/sparc/math-emu/math_32.c

308

case FDTOQ: TYPE(3,3,1,2,1,0,0); break;

arch/sparc/math-emu/math_32.c

309

case FQTOI: TYPE(3,1,0,3,1,0,0); break;

arch/sparc/math-emu/math_32.c

310

case FSQRTS: TYPE(2,1,1,1,1,0,0); break;

arch/sparc/math-emu/math_32.c

311

case FSQRTD: TYPE(2,2,1,2,1,0,0); break;

arch/sparc/math-emu/math_32.c

315

case FDIVD: TYPE(2,2,1,2,1,2,1); break;

arch/sparc/math-emu/math_32.c

319

case FDIVS: TYPE(2,1,1,1,1,1,1); break;

arch/sparc/math-emu/math_32.c

320

case FSMULD: TYPE(2,2,1,1,1,1,1); break;

arch/sparc/math-emu/math_32.c

321

case FDTOS: TYPE(2,1,1,2,1,0,0); break;

arch/sparc/math-emu/math_32.c

322

case FSTOD: TYPE(2,2,1,1,1,0,0); break;

arch/sparc/math-emu/math_32.c

323

case FSTOI: TYPE(2,1,0,1,1,0,0); break;

arch/sparc/math-emu/math_32.c

324

case FDTOI: TYPE(2,1,0,2,1,0,0); break;

arch/sparc/math-emu/math_32.c

325

case FITOS: TYPE(2,1,1,1,0,0,0); break;

arch/sparc/math-emu/math_32.c

326

case FITOD: TYPE(2,2,1,1,0,0,0); break;

arch/sparc/math-emu/math_32.c

329

case FNEGS: TYPE(2,1,0,1,0,0,0); break;

arch/sparc/math-emu/math_32.c

333

case FCMPS: TYPE(3,0,0,1,1,1,1); break;

arch/sparc/math-emu/math_32.c

334

case FCMPES: TYPE(3,0,0,1,1,1,1); break;

arch/sparc/math-emu/math_32.c

335

case FCMPD: TYPE(3,0,0,2,1,2,1); break;

arch/sparc/math-emu/math_32.c

336

case FCMPED: TYPE(3,0,0,2,1,2,1); break;

arch/sparc/math-emu/math_32.c

337

case FCMPQ: TYPE(3,0,0,3,1,3,1); break;

arch/sparc/math-emu/math_32.c

338

case FCMPEQ: TYPE(3,0,0,3,1,3,1); break;

arch/sparc/math-emu/math_64.c

198

case FABSQ: TYPE(3,3,0,3,0,0,0); break;

arch/sparc/math-emu/math_64.c

199

case FSQRTQ: TYPE(3,3,1,3,1,0,0); break;

arch/sparc/math-emu/math_64.c

203

case FDIVQ: TYPE(3,3,1,3,1,3,1); break;

arch/sparc/math-emu/math_64.c

204

case FDMULQ: TYPE(3,3,1,2,1,2,1); break;

arch/sparc/math-emu/math_64.c

205

case FQTOX: TYPE(3,2,0,3,1,0,0); break;

arch/sparc/math-emu/math_64.c

206

case FXTOQ: TYPE(3,3,1,2,0,0,0); break;

arch/sparc/math-emu/math_64.c

207

case FQTOS: TYPE(3,1,1,3,1,0,0); break;

arch/sparc/math-emu/math_64.c

208

case FQTOD: TYPE(3,2,1,3,1,0,0); break;

arch/sparc/math-emu/math_64.c

209

case FITOQ: TYPE(3,3,1,1,0,0,0); break;

arch/sparc/math-emu/math_64.c

210

case FSTOQ: TYPE(3,3,1,1,1,0,0); break;

arch/sparc/math-emu/math_64.c

211

case FDTOQ: TYPE(3,3,1,2,1,0,0); break;

arch/sparc/math-emu/math_64.c

212

case FQTOI: TYPE(3,1,0,3,1,0,0); break;

arch/sparc/math-emu/math_64.c

223

TYPE(x,1,1,1,1,0,0);

arch/sparc/math-emu/math_64.c

231

TYPE(x,2,1,2,1,0,0);

arch/sparc/math-emu/math_64.c

239

case FDIVD: TYPE(2,2,1,2,1,2,1); break;

arch/sparc/math-emu/math_64.c

243

case FDIVS: TYPE(2,1,1,1,1,1,1); break;

arch/sparc/math-emu/math_64.c

244

case FSMULD: TYPE(2,2,1,1,1,1,1); break;

arch/sparc/math-emu/math_64.c

245

case FSTOX: TYPE(2,2,0,1,1,0,0); break;

arch/sparc/math-emu/math_64.c

246

case FDTOX: TYPE(2,2,0,2,1,0,0); break;

arch/sparc/math-emu/math_64.c

247

case FDTOS: TYPE(2,1,1,2,1,0,0); break;

arch/sparc/math-emu/math_64.c

248

case FSTOD: TYPE(2,2,1,1,1,0,0); break;

arch/sparc/math-emu/math_64.c

249

case FSTOI: TYPE(2,1,0,1,1,0,0); break;

arch/sparc/math-emu/math_64.c

250

case FDTOI: TYPE(2,1,0,2,1,0,0); break;

arch/sparc/math-emu/math_64.c

253

case FXTOS: TYPE(2,1,1,2,0,0,0); break;

arch/sparc/math-emu/math_64.c

254

case FXTOD: TYPE(2,2,1,2,0,0,0); break;

arch/sparc/math-emu/math_64.c

256

case FITOS: TYPE(2,1,1,1,0,0,0); break;

arch/sparc/math-emu/math_64.c

258

case FITOD: TYPE(2,2,1,1,0,0,0); break;

arch/sparc/math-emu/math_64.c

264

case FCMPQ: TYPE(3,0,0,3,1,3,1); break;

arch/sparc/math-emu/math_64.c

265

case FCMPEQ: TYPE(3,0,0,3,1,3,1); break;

arch/sparc/math-emu/math_64.c

354

TYPE(3,3,0,3,0,0,0);

arch/x86/kernel/fpu/init.c

146

#define CHECK_MEMBER_AT_END_OF(TYPE, MEMBER) \

arch/x86/kernel/fpu/init.c

147

BUILD_BUG_ON(sizeof(TYPE) != \

arch/x86/kernel/fpu/init.c

148

ALIGN(offsetofend(TYPE, MEMBER), _Alignof(TYPE)))

drivers/block/null_blk/main.c

344

#define NULLB_DEVICE_ATTR(NAME, TYPE, APPLY) \

drivers/block/null_blk/main.c

348

return nullb_device_##TYPE##_attr_show( \

drivers/block/null_blk/main.c

355

int (*apply_fn)(struct nullb_device *dev, TYPE new_value) = APPLY;\

drivers/block/null_blk/main.c

357

TYPE new_value = 0; \

drivers/block/null_blk/main.c

360

ret = nullb_device_##TYPE##_attr_store(&new_value, page, count);\

drivers/gpib/gpio/gpib_bitbang.c

32

#define ENABLE_IRQ(IRQ, TYPE) irq_set_irq_type(IRQ, TYPE)

drivers/gpu/drm/amd/amdkfd/kfd_int_process_v11.c

203

TYPE),

drivers/gpu/drm/amd/amdkfd/kfd_int_process_v11.c

396

SQ_INTERRUPT_WORD_ERROR_CTXID0, TYPE);

drivers/gpu/drm/amd/amdkfd/kfd_int_process_v12_1.c

174

REG_GET_FIELD(context_id0, SQ_INTERRUPT_WORD_ERROR_CTXID0, TYPE),

drivers/gpu/drm/amd/amdkfd/kfd_int_process_v12_1.c

369

SQ_INTERRUPT_WORD_ERROR_CTXID0, TYPE);

drivers/gpu/drm/nouveau/nouveau_bo5039.c

124

NVDEF(NV5039, BUFFER_NOTIFY, TYPE, WRITE_ONLY));

drivers/gpu/drm/nouveau/nvkm/subdev/fsp/gh100.c

182

if (NVDEF_TEST(reply.nvdm_header, MCTP, MSG_HEADER, TYPE, !=, VENDOR_PCI) ||

drivers/gpu/drm/nouveau/nvkm/subdev/fsp/gh100.c

219

msg.nvdm_header = NVDEF(MCTP, MSG_HEADER, TYPE, VENDOR_PCI) |

drivers/gpu/drm/radeon/mkregtable.c

20

#define offsetof(TYPE, MEMBER) ((size_t) &((TYPE *)0)->MEMBER)

drivers/gpu/drm/xe/xe_gt_sriov_pf_debugfs.c

115

#define DEFINE_SRIOV_GT_POLICY_DEBUGFS_ATTRIBUTE(POLICY, TYPE, FORMAT) \

drivers/gpu/drm/xe/xe_gt_sriov_pf_debugfs.c

123

if (val > (TYPE)~0ull) \

drivers/gpu/drm/xe/xe_gt_sriov_pf_debugfs.c

472

#define DEFINE_SRIOV_GT_CONFIG_DEBUGFS_ATTRIBUTE(CONFIG, TYPE, FORMAT) \

drivers/gpu/drm/xe/xe_gt_sriov_pf_debugfs.c

481

if (val > (TYPE)~0ull) \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

115

#define DEFINE_SIMPLE_BULK_PROVISIONING_SRIOV_DEV_ATTR_WO(NAME, ITEM, TYPE) \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

120

TYPE value; \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

123

err = kstrto##TYPE(buf, 0, &value); \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

199

#define DEFINE_SIMPLE_PROVISIONING_SRIOV_VF_ATTR(NAME, ITEM, TYPE, FORMAT) \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

203

TYPE value = 0; \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

216

TYPE value; \

drivers/gpu/drm/xe/xe_sriov_pf_sysfs.c

219

err = kstrto##TYPE(buf, 0, &value); \

drivers/gpu/drm/xe/xe_tile_sriov_pf_debugfs.c

131

#define DEFINE_SRIOV_TILE_CONFIG_DEBUGFS_ATTRIBUTE(NAME, CONFIG, TYPE, FORMAT) \

drivers/gpu/drm/xe/xe_tile_sriov_pf_debugfs.c

141

if (val > (TYPE)~0ull) \

drivers/infiniband/hw/hfi1/file_ops.c

133

HFI1_MMAP_TOKEN_SET(TYPE, type) | \

drivers/infiniband/hw/hfi1/file_ops.c

341

type = HFI1_MMAP_TOKEN_GET(TYPE, token);

drivers/md/dm-vdo/memory-alloc.h

70

#define vdo_allocate(COUNT, TYPE, WHAT, PTR) \

drivers/md/dm-vdo/memory-alloc.h

71

__vdo_do_allocation(COUNT, sizeof(TYPE), 0, __alignof__(TYPE), WHAT, PTR)

drivers/net/ethernet/cavium/liquidio/octeon_device.h

627

#define CHIP_CONF(oct, TYPE) \

drivers/net/ethernet/cavium/liquidio/octeon_device.h

628

(((struct octeon_ ## TYPE *)((oct)->chip))->conf)

drivers/net/ethernet/huawei/hinic/hinic_hw_cmdq.c

641

enum hinic_cmdq_type cmdq_type = CMDQ_CEQE_GET(ceqe_data, TYPE);

drivers/net/ethernet/huawei/hinic/hinic_hw_eqs.c

242

event = HINIC_EQ_ELEM_DESC_GET(aeqe_desc, TYPE);

drivers/net/ethernet/huawei/hinic/hinic_hw_qp.c

622

HINIC_SQ_DB_INFO_SET(HINIC_DB_SQ_TYPE, TYPE) |

drivers/net/ethernet/huawei/hinic3/hinic3_cmdq.c

234

enum hinic3_cmdq_type cmdq_type = CMDQ_CEQE_GET(ceqe_data, TYPE);

drivers/net/ethernet/huawei/hinic3/hinic3_eqs.c

217

event = EQ_ELEM_DESC_GET(aeqe, TYPE);

drivers/net/ethernet/huawei/hinic3/hinic3_nic_io.h

88

cpu_to_le32(DB_INFO_SET(DB_SRC_TYPE, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

1355

switch (FM10K_MSG_HDR_FIELD_GET(mbx->mbx_hdr, TYPE)) {

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

840

mbx->mbx_hdr = FM10K_MSG_HDR_FIELD_SET(FM10K_MSG_CONNECT, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

853

u32 hdr = FM10K_MSG_HDR_FIELD_SET(FM10K_MSG_DATA, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

879

u32 hdr = FM10K_MSG_HDR_FIELD_SET(FM10K_MSG_DISCONNECT, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

900

u32 hdr = FM10K_MSG_HDR_FIELD_SET(FM10K_MSG_DISCONNECT, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

937

mbx->mbx_hdr = FM10K_MSG_HDR_FIELD_SET(FM10K_MSG_ERROR, TYPE) |

drivers/net/ethernet/intel/fm10k/fm10k_mbx.c

955

type = FM10K_MSG_HDR_FIELD_GET(*hdr, TYPE);

drivers/net/netdevsim/hwstats.c

384

#define NSIM_DEV_HWSTATS_FOPS(ACTION, TYPE) \

drivers/net/netdevsim/hwstats.c

387

.type = TYPE, \

drivers/net/wireless/rsi/rsi_sdio.h

70

#define RSI_GET_SDIO_INTERRUPT_TYPE(_I, TYPE) \

drivers/net/wireless/rsi/rsi_sdio.h

72

TYPE = \

drivers/pinctrl/cirrus/pinctrl-lochnagar.c

440

#define LN_FUNC(NAME, TYPE, OP) \

drivers/pinctrl/cirrus/pinctrl-lochnagar.c

441

{ .name = NAME, .type = LN_FTYPE_##TYPE, .op = OP }

drivers/power/supply/power_supply_sysfs.c

217

POWER_SUPPLY_ENUM_ATTR(TYPE),

drivers/staging/nvec/nvec_power.c

106

MANUFACTURER, MODEL, TYPE,

drivers/staging/nvec/nvec_power.c

203

case TYPE:

fs/jfs/jfs_btree.h

142

#define BT_GETSEARCH(IP, LEAF, BN, MP, TYPE, P, INDEX, ROOT)\

fs/jfs/jfs_btree.h

147

P = (TYPE *)MP->data;\

fs/jfs/jfs_btree.h

149

P = (TYPE *)&JFS_IP(IP)->ROOT;\

fs/jfs/jfs_btree.h

50

#define BT_PAGE(IP, MP, TYPE, ROOT)\

fs/jfs/jfs_btree.h

51

(BT_IS_ROOT(MP) ? (TYPE *)&JFS_IP(IP)->ROOT : (TYPE *)(MP)->data)

fs/jfs/jfs_btree.h

54

#define BT_GETPAGE(IP, BN, MP, TYPE, SIZE, P, RC, ROOT)\

fs/jfs/jfs_btree.h

59

P = (TYPE *)&JFS_IP(IP)->ROOT;\

include/acpi/actypes.h

1327

#define ACPI_FLEX_ARRAY(TYPE, NAME) TYPE NAME[0]

include/acpi/platform/acgcc.h

69

#define ACPI_FLEX_ARRAY(TYPE, NAME) \

include/acpi/platform/acgcc.h

72

TYPE NAME[]; \

include/linux/cache.h

151

#define CACHELINE_ASSERT_GROUP_MEMBER(TYPE, GROUP, MEMBER) \

include/linux/cache.h

152

BUILD_BUG_ON(!(offsetof(TYPE, MEMBER) >= \

include/linux/cache.h

153

offsetofend(TYPE, __cacheline_group_begin__##GROUP) && \

include/linux/cache.h

154

offsetofend(TYPE, MEMBER) <= \

include/linux/cache.h

155

offsetof(TYPE, __cacheline_group_end__##GROUP)))

include/linux/cache.h

159

#define CACHELINE_ASSERT_GROUP_SIZE(TYPE, GROUP, SIZE) \

include/linux/cache.h

160

BUILD_BUG_ON(offsetof(TYPE, __cacheline_group_end__##GROUP) - \

include/linux/cache.h

161

offsetofend(TYPE, __cacheline_group_begin__##GROUP) > \

include/linux/filter.h

151

#define BPF_ENDIAN(TYPE, DST, LEN) \

include/linux/filter.h

153

.code = BPF_ALU | BPF_END | BPF_SRC(TYPE), \

include/linux/filter.h

290

#define BPF_MOV64_RAW(TYPE, DST, SRC, IMM) \

include/linux/filter.h

292

.code = BPF_ALU64 | BPF_MOV | BPF_SRC(TYPE), \

include/linux/filter.h

298

#define BPF_MOV32_RAW(TYPE, DST, SRC, IMM) \

include/linux/filter.h

300

.code = BPF_ALU | BPF_MOV | BPF_SRC(TYPE), \

include/linux/filter.h

632

#define bpf_ctx_range(TYPE, MEMBER) \

include/linux/filter.h

633

offsetof(TYPE, MEMBER) ... offsetofend(TYPE, MEMBER) - 1

include/linux/filter.h

634

#define bpf_ctx_range_till(TYPE, MEMBER1, MEMBER2) \

include/linux/filter.h

635

offsetof(TYPE, MEMBER1) ... offsetofend(TYPE, MEMBER2) - 1

include/linux/filter.h

637

# define bpf_ctx_range_ptr(TYPE, MEMBER) \

include/linux/filter.h

638

offsetof(TYPE, MEMBER) ... offsetofend(TYPE, MEMBER) - 1

include/linux/filter.h

640

# define bpf_ctx_range_ptr(TYPE, MEMBER) \

include/linux/filter.h

641

offsetof(TYPE, MEMBER) ... offsetof(TYPE, MEMBER) + 8 - 1

include/linux/filter.h

644

#define bpf_target_off(TYPE, MEMBER, SIZE, PTR_SIZE) \

include/linux/filter.h

646

BUILD_BUG_ON(sizeof_field(TYPE, MEMBER) != (SIZE)); \

include/linux/filter.h

648

offsetof(TYPE, MEMBER); \

include/linux/firmware/thead/thead,th1520-aon.h

96

#define RPC_SET_SVC_FLAG_MSG_TYPE(MESG, TYPE) ((MESG)->svc |= (TYPE) << 7)

include/linux/fs_parser.h

107

#define __fsparam(TYPE, NAME, OPT, FLAGS, DATA) \

include/linux/fs_parser.h

111

.type = TYPE, \

include/linux/overflow.h

535

#define DEFINE_FLEX(TYPE, NAME, MEMBER, COUNTER, COUNT) \

include/linux/overflow.h

536

_DEFINE_FLEX(TYPE, NAME, MEMBER, COUNT, = { .COUNTER = COUNT, })

include/linux/overflow.h

572

#define overflows_flex_counter_type(TYPE, FAM, COUNT) \

include/linux/overflow.h

573

(overflows_type(COUNT, typeof_flex_counter(((TYPE *)NULL)->FAM)))

include/linux/slab.h

971

#define __alloc_objs(KMALLOC, GFP, TYPE, COUNT) \

include/linux/slab.h

973

const size_t __obj_size = size_mul(sizeof(TYPE), COUNT); \

include/linux/slab.h

974

(TYPE *)KMALLOC(__obj_size, GFP); \

include/linux/slab.h

990

#define __alloc_flex(KMALLOC, GFP, TYPE, FAM, COUNT) \

include/linux/slab.h

993

const size_t __obj_size = struct_size_t(TYPE, FAM, __count); \

include/linux/slab.h

994

TYPE *__obj_ptr = KMALLOC(__obj_size, GFP); \

include/linux/stddef.h

109

#define __TRAILING_OVERLAP(TYPE, NAME, FAM, ATTRS, MEMBERS) \

include/linux/stddef.h

111

TYPE NAME; \

include/linux/stddef.h

113

unsigned char __offset_to_FAM[offsetof(TYPE, FAM)]; \

include/linux/stddef.h

129

#define TRAILING_OVERLAP(TYPE, NAME, FAM, MEMBERS) \

include/linux/stddef.h

130

__TRAILING_OVERLAP(TYPE, NAME, FAM, /* no attrs */, MEMBERS)

include/linux/stddef.h

16

#define offsetof(TYPE, MEMBER) __builtin_offsetof(TYPE, MEMBER)

include/linux/stddef.h

24

#define sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

include/linux/stddef.h

32

#define offsetofend(TYPE, MEMBER) \

include/linux/stddef.h

33

(offsetof(TYPE, MEMBER) + sizeof_field(TYPE, MEMBER))

include/linux/stddef.h

93

#define DECLARE_FLEX_ARRAY(TYPE, NAME) \

include/linux/stddef.h

94

__DECLARE_FLEX_ARRAY(TYPE, NAME)

include/uapi/linux/stddef.h

56

#define __DECLARE_FLEX_ARRAY(TYPE, NAME) \

include/uapi/linux/stddef.h

59

TYPE NAME[]; \

lib/crc/mips/crc32.h

16

#define _ASM_SET_CRC(OP, SZ, TYPE) \

lib/crc/mips/crc32.h

22

((SZ) << 6) | ((TYPE) << 8)) \

lib/crc/mips/crc32.h

24

((SZ) << 14) | ((TYPE) << 3)))

lib/crc/mips/crc32.h

25

#define _ASM_UNSET_CRC(op, SZ, TYPE) ".purgem " #op "\n\t"

lib/crc/mips/crc32.h

27

#define _ASM_SET_CRC(op, SZ, TYPE) ".set\tcrc\n\t"

lib/crc/mips/crc32.h

28

#define _ASM_UNSET_CRC(op, SZ, TYPE)

lib/crc/mips/crc32.h

31

#define __CRC32(crc, value, op, SZ, TYPE) \

lib/crc/mips/crc32.h

35

_ASM_SET_CRC(op, SZ, TYPE) \

lib/crc/mips/crc32.h

37

_ASM_UNSET_CRC(op, SZ, TYPE) \

lib/fault-inject.c

361

#define FAULT_CONFIGFS_ATTR_NAMED(NAME, ATTR_NAME, MEMBER, TYPE) \

lib/fault-inject.c

364

return fault_##TYPE##_attr_show(to_fault_config(item)->attr.MEMBER, page); \

lib/fault-inject.c

369

return fault_##TYPE##_attr_store(&config->attr.MEMBER, page, count); \

lib/fault-inject.c

373

#define FAULT_CONFIGFS_ATTR(NAME, TYPE) \

lib/fault-inject.c

374

FAULT_CONFIGFS_ATTR_NAMED(NAME, __stringify(NAME), NAME, TYPE)

lib/zlib_inflate/inffast.c

300

state->mode = TYPE;

lib/zlib_inflate/inflate.c

173

state->mode = TYPE;

lib/zlib_inflate/inflate.c

358

if (state->mode == TYPE) state->mode = TYPEDO; /* skip check */

lib/zlib_inflate/inflate.c

391

state->mode = hold & 0x200 ? DICTID : TYPE;

lib/zlib_inflate/inflate.c

406

state->mode = TYPE;

lib/zlib_inflate/inflate.c

408

case TYPE:

lib/zlib_inflate/inflate.c

464

state->mode = TYPE;

lib/zlib_inflate/inflate.c

608

state->mode = TYPE;

lib/zlib_inflate/inflate.c

758

(state->mode == TYPE ? 128 : 0);

lib/zlib_inflate/inflate.c

791

if (state->mode != TYPE && state->mode != HEAD)

net/core/filter.c

10673

#define SOCK_OPS_GET_OR_SET_FIELD(BPF_FIELD, OBJ_FIELD, OBJ, TYPE) \

net/core/filter.c

10675

if (TYPE == BPF_WRITE) \

net/mac80211/s1g.c

17

STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_S1G);

net/mac80211/sta_info.c

2519

switch (STA_STATS_GET(TYPE, rate)) {

net/mac80211/sta_info.h

1079

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_VHT);

net/mac80211/sta_info.h

1084

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_HT);

net/mac80211/sta_info.h

1088

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_LEGACY);

net/mac80211/sta_info.h

1093

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_HE);

net/mac80211/sta_info.h

1101

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_EHT);

net/mac80211/sta_info.h

1108

r |= STA_STATS_FIELD(TYPE, STA_STATS_RATE_TYPE_UHR);

net/netfilter/x_tables.c

307

#define XT_OBJ_TO_USER(U, K, TYPE, C_SIZE) \

net/netfilter/x_tables.c

308

xt_obj_to_user(&U->u.TYPE##_size, C_SIZE ? : K->u.TYPE##_size, \

net/netfilter/x_tables.c

309

U->u.user.name, K->u.kernel.TYPE->name, \

net/netfilter/x_tables.c

310

&U->u.user.revision, K->u.kernel.TYPE->revision)

net/netfilter/x_tables.c

326

#define XT_DATA_TO_USER(U, K, TYPE) \

net/netfilter/x_tables.c

328

K->u.kernel.TYPE->usersize, \

net/netfilter/x_tables.c

329

K->u.kernel.TYPE->TYPE##size, \

net/netfilter/x_tables.c

330

XT_ALIGN(K->u.kernel.TYPE->TYPE##size))

net/netfilter/x_tables.c

789

#define COMPAT_XT_DATA_TO_USER(U, K, TYPE, C_SIZE) \

net/netfilter/x_tables.c

791

K->u.kernel.TYPE->usersize, \

samples/bpf/test_lru_dist.c

25

# define offsetof(TYPE, MEMBER) ((size_t)&((TYPE *)0)->MEMBER)

scripts/gcc-plugins/gcc-common.h

101

#define C_TYPE_FIELDS_READONLY(TYPE) TREE_LANG_FLAG_1(TYPE)

scripts/genksyms/parse.y

112

%token TYPE

scripts/genksyms/parse.y

276

| TYPE { (*$1)->tag = SYM_TYPEDEF; $$ = $1; }

tools/include/linux/filter.h

134

#define BPF_MOV64_RAW(TYPE, DST, SRC, IMM) \

tools/include/linux/filter.h

136

.code = BPF_ALU64 | BPF_MOV | BPF_SRC(TYPE), \

tools/include/linux/filter.h

142

#define BPF_MOV32_RAW(TYPE, DST, SRC, IMM) \

tools/include/linux/filter.h

144

.code = BPF_ALU | BPF_MOV | BPF_SRC(TYPE), \

tools/include/linux/filter.h

70

#define BPF_ENDIAN(TYPE, DST, LEN) \

tools/include/linux/filter.h

72

.code = BPF_ALU | BPF_END | BPF_SRC(TYPE), \

tools/include/linux/kernel.h

26

#define offsetof(TYPE, MEMBER) ((size_t) &((TYPE *)0)->MEMBER)

tools/include/linux/slab.h

205

#define __alloc_objs(KMALLOC, GFP, TYPE, COUNT) \

tools/include/linux/slab.h

207

const size_t __obj_size = size_mul(sizeof(TYPE), COUNT); \

tools/include/linux/slab.h

208

(TYPE *)KMALLOC(__obj_size, GFP); \

tools/include/nolibc/stddef.h

21

#define offsetof(TYPE, FIELD) ((size_t) &((TYPE *)0)->FIELD)

tools/include/nolibc/types.h

160

#define container_of(PTR, TYPE, FIELD) ({ \

tools/include/nolibc/types.h

161

__typeof__(((TYPE *)0)->FIELD) *__FIELD_PTR = (PTR); \

tools/include/nolibc/types.h

162

(TYPE *)((char *) __FIELD_PTR - offsetof(TYPE, FIELD)); \

tools/include/uapi/linux/stddef.h

49

#define __DECLARE_FLEX_ARRAY(TYPE, NAME) \

tools/include/uapi/linux/stddef.h

52

TYPE NAME[]; \

tools/lib/bpf/libbpf_common.h

64

#define LIBBPF_OPTS(TYPE, NAME, ...) \

tools/lib/bpf/libbpf_common.h

65

struct TYPE NAME = ({ \

tools/lib/bpf/libbpf_common.h

66

memset(&NAME, 0, sizeof(struct TYPE)); \

tools/lib/bpf/libbpf_common.h

67

(struct TYPE) { \

tools/lib/bpf/libbpf_common.h

68

.sz = sizeof(struct TYPE), \

tools/lib/bpf/libbpf_internal.h

110

# define offsetofend(TYPE, FIELD) \

tools/lib/bpf/libbpf_internal.h

111

(offsetof(TYPE, FIELD) + sizeof(((TYPE *)0)->FIELD))

tools/lib/bpf/skel_internal.h

225

#define offsetofend(TYPE, MEMBER) \

tools/lib/bpf/skel_internal.h

226

(offsetof(TYPE, MEMBER) + sizeof((((TYPE *)0)->MEMBER)))

tools/objtool/klp-diff.c

24

#define sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

tools/testing/selftests/bpf/bpf_util.h

74

#define sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

tools/testing/selftests/bpf/bpf_util.h

78

#define offsetofend(TYPE, MEMBER) \

tools/testing/selftests/bpf/bpf_util.h

79

(offsetof(TYPE, MEMBER) + sizeof_field(TYPE, MEMBER))

tools/testing/selftests/bpf/prog_tests/sk_assign.c

211

#define TEST(NAME, FAMILY, TYPE, REWRITE) \

tools/testing/selftests/bpf/prog_tests/sk_assign.c

218

.type = TYPE, \

tools/testing/selftests/bpf/progs/bpf_misc.h

183

#define sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

tools/testing/selftests/bpf/progs/bpf_misc.h

184

#define offsetofend(TYPE, MEMBER) \

tools/testing/selftests/bpf/progs/bpf_misc.h

185

(offsetof(TYPE, MEMBER) + sizeof_field(TYPE, MEMBER))

tools/testing/selftests/bpf/progs/test_cls_redirect_dynptr.c

28

#define offsetofend(TYPE, MEMBER) \

tools/testing/selftests/bpf/progs/test_cls_redirect_dynptr.c

29

(offsetof(TYPE, MEMBER) + sizeof((((TYPE *)0)->MEMBER)))

tools/testing/selftests/bpf/progs/test_pkt_md_access.c

11

#define TEST_FIELD(TYPE, FIELD, MASK) \

tools/testing/selftests/bpf/progs/test_pkt_md_access.c

13

TYPE tmp = *(volatile TYPE *)&skb->FIELD; \

tools/testing/selftests/bpf/progs/test_pkt_md_access.c

19

#define TEST_FIELD(TYPE, FIELD, MASK) \

tools/testing/selftests/bpf/progs/test_pkt_md_access.c

21

TYPE tmp = *((volatile TYPE *)&skb->FIELD + \

tools/testing/selftests/bpf/progs/test_pkt_md_access.c

22

TEST_FIELD_OFFSET(skb->FIELD, TYPE)); \

tools/testing/selftests/bpf/progs/test_select_reuseport_kern.c

18

#define offsetof(TYPE, MEMBER) ((size_t) &((TYPE *)0)->MEMBER)

tools/testing/selftests/iommu/iommufd_utils.h

55

#define sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

tools/testing/selftests/iommu/iommufd_utils.h

56

#define offsetofend(TYPE, MEMBER) \

tools/testing/selftests/iommu/iommufd_utils.h

57

(offsetof(TYPE, MEMBER) + sizeof_field(TYPE, MEMBER))

tools/testing/selftests/kvm/arm64/set_id_regs.c

47

#define __REG_FTR_BITS(NAME, SIGNED, TYPE, SHIFT, MASK, SAFE_VAL) \

tools/testing/selftests/kvm/arm64/set_id_regs.c

51

.type = TYPE, \

tools/testing/selftests/kvm/guest_print_test.c

28

TYPE(test_type_i64, I64, "%ld", int64_t) \

tools/testing/selftests/kvm/guest_print_test.c

29

TYPE(test_type_u64, U64u, "%lu", uint64_t) \

tools/testing/selftests/kvm/guest_print_test.c

30

TYPE(test_type_x64, U64x, "0x%lx", uint64_t) \

tools/testing/selftests/kvm/guest_print_test.c

31

TYPE(test_type_X64, U64X, "0x%lX", uint64_t) \

tools/testing/selftests/kvm/guest_print_test.c

32

TYPE(test_type_u32, U32u, "%u", uint32_t) \

tools/testing/selftests/kvm/guest_print_test.c

33

TYPE(test_type_x32, U32x, "0x%x", uint32_t) \

tools/testing/selftests/kvm/guest_print_test.c

34

TYPE(test_type_X32, U32X, "0x%X", uint32_t) \

tools/testing/selftests/kvm/guest_print_test.c

35

TYPE(test_type_int, INT, "%d", int) \

tools/testing/selftests/kvm/guest_print_test.c

36

TYPE(test_type_char, CHAR, "%c", char) \

tools/testing/selftests/kvm/guest_print_test.c

37

TYPE(test_type_str, STR, "'%s'", const char *) \

tools/testing/selftests/kvm/guest_print_test.c

38

TYPE(test_type_ptr, PTR, "%p", uintptr_t)

tools/testing/selftests/net/ipsec.c

47

#define offsetof(TYPE, MEMBER) __builtin_offsetof(TYPE, MEMBER)

tools/testing/selftests/rseq/rseq.h

24

#define rseq_sizeof_field(TYPE, MEMBER) sizeof((((TYPE *)0)->MEMBER))

tools/testing/selftests/rseq/rseq.h

28

#define rseq_offsetofend(TYPE, MEMBER) \

tools/testing/selftests/rseq/rseq.h

29

(offsetof(TYPE, MEMBER) + rseq_sizeof_field(TYPE, MEMBER))

tools/testing/selftests/ublk/utils.h

12

#define offsetof(TYPE, MEMBER) ((size_t)&((TYPE *)0)->MEMBER)

tools/usb/usbip/libsrc/list.h

124

#define offsetof(TYPE, MEMBER) ((size_t) &((TYPE *)0)->MEMBER)