https://github.com/AnkitDubeycs25 created https://github.com/llvm/llvm-project/pull/169648
This is my first commit. Requesting reviews. >From 738a2111fdc5f56d3f5f53a9d3a05fed689b74f3 Mon Sep 17 00:00:00 2001 From: AnkitDubeycs25 <[email protected]> Date: Wed, 26 Nov 2025 18:17:45 +0530 Subject: [PATCH] [CIR][CIRGen][Builtin][X86] Compress Store Intrinsics This is my first commit. Requesting reviews. --- clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp | 16 +++++++++++++++- .../test/CIR/CodeGen/X86/compressStore_builtin.c | 5 +++++ 2 files changed, 20 insertions(+), 1 deletion(-) create mode 100644 clang/test/CIR/CodeGen/X86/compressStore_builtin.c diff --git a/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp b/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp index e7aa8a234efd9..5c3e7f7512851 100644 --- a/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp +++ b/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp @@ -90,6 +90,14 @@ static mlir::Value getMaskVecValue(CIRGenFunction &cgf, const CallExpr *expr, return maskVec; } +static mlir::Value emitX86CompressStore(CIRGenFunction &cgf, const CallExpr *expr, ArrayRef<mlir::Value> ops){ + auto ResultTy = cast<cir::VectorType>(ops[1].getType()); + mlir::Value MaskValue = getMaskVecValue(cgf, expr, ops[2], cast<cir::VectorType>(ResultTy).getSize()); + mlir::Value ptr = ops[0]; + + return emitIntrinsicCallOp(cgf, expr, "masked_compressstore", ResultTy, llvm::SmallVector<mlir::Value, 3>{ops[1], ptr, MaskValue}); + +} mlir::Value CIRGenFunction::emitX86BuiltinExpr(unsigned builtinID, const CallExpr *expr) { if (builtinID == Builtin::BI__builtin_cpu_is) { @@ -400,7 +408,12 @@ mlir::Value CIRGenFunction::emitX86BuiltinExpr(unsigned builtinID, case X86::BI__builtin_ia32_expandloadhi512_mask: case X86::BI__builtin_ia32_expandloadqi128_mask: case X86::BI__builtin_ia32_expandloadqi256_mask: - case X86::BI__builtin_ia32_expandloadqi512_mask: + case X86::BI__builtin_ia32_expandloadqi512_mask:{ + cgm.errorNYI(expr->getSourceRange(), + std::string("unimplemented X86 builtin call: ") + + getContext().BuiltinInfo.getName(builtinID)); + return {}; + } case X86::BI__builtin_ia32_compressstoredf128_mask: case X86::BI__builtin_ia32_compressstoredf256_mask: case X86::BI__builtin_ia32_compressstoredf512_mask: @@ -419,6 +432,7 @@ mlir::Value CIRGenFunction::emitX86BuiltinExpr(unsigned builtinID, case X86::BI__builtin_ia32_compressstoreqi128_mask: case X86::BI__builtin_ia32_compressstoreqi256_mask: case X86::BI__builtin_ia32_compressstoreqi512_mask: + return emitX86CompressStore(*this, expr, ops); case X86::BI__builtin_ia32_expanddf128_mask: case X86::BI__builtin_ia32_expanddf256_mask: case X86::BI__builtin_ia32_expanddf512_mask: diff --git a/clang/test/CIR/CodeGen/X86/compressStore_builtin.c b/clang/test/CIR/CodeGen/X86/compressStore_builtin.c new file mode 100644 index 0000000000000..1407e21428aee --- /dev/null +++ b/clang/test/CIR/CodeGen/X86/compressStore_builtin.c @@ -0,0 +1,5 @@ +#include <immintrin.h> + +void test_compress_store(void *__P, __mmask8 __U, __m128d __A){ + return _mm_mask_compressstoreu_pd (__P, __U, __A); +} \ No newline at end of file _______________________________________________ cfe-commits mailing list [email protected] https://lists.llvm.org/cgi-bin/mailman/listinfo/cfe-commits
