[clang] [CIR][CIRGen][Builtin][X86] Multishift Intrinsics (PR #169618)

[Omkar Rasal via cfe-commits]

https://github.com/cs25mtech12008 updated https://github.com/llvm/llvm-project/pull/169618

>From 397436e9a63ceb5b111a2f63038b7d5922407347 Mon Sep 17 00:00:00 2001
From: cs25mtech12008 <cs25mtech12008 at iith.ac.in>
Date: Wed, 26 Nov 2025 12:47:53 +0530
Subject: [PATCH] [CIR][CIRGen][Builtin][X86] Multishift Intrinsics

Added builtin support for the multishift operation with test file.

changes has been done in CIRGenBuiltinX86 file
---
 clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp    |  7 ++++++
 .../CIR/CodeGen/X86/avx512vbmi-builtins.c     | 22 +++++++++++++++++++
 2 files changed, 29 insertions(+)
 create mode 100644 clang/test/CIR/CodeGen/X86/avx512vbmi-builtins.c

diff --git a/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp b/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp
index e7aa8a234efd9..4cbeecf0d8ea3 100644
--- a/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp
+++ b/clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp
@@ -877,9 +877,16 @@ mlir::Value CIRGenFunction::emitX86BuiltinExpr(unsigned builtinID,
   case X86::BI__builtin_ia32_vp2intersect_d_512:
   case X86::BI__builtin_ia32_vp2intersect_d_256:
   case X86::BI__builtin_ia32_vp2intersect_d_128:
+    cgm.errorNYI(expr->getSourceRange(),
+                 std::string("unimplemented X86 builtin call: ") +
+                     getContext().BuiltinInfo.getName(builtinID));
+    return {};
   case X86::BI__builtin_ia32_vpmultishiftqb128:
+    return emitIntrinsicCallOp(*this, expr, "x86_avx512_pmultishift_qb_128", ops[0].getType(), ops);
   case X86::BI__builtin_ia32_vpmultishiftqb256:
+    return emitIntrinsicCallOp(*this, expr, "x86_avx512_pmultishift_qb_256", ops[0].getType(), ops);
   case X86::BI__builtin_ia32_vpmultishiftqb512:
+    return emitIntrinsicCallOp(*this, expr, "x86_avx512_pmultishift_qb_512", ops[0].getType(), ops);
   case X86::BI__builtin_ia32_vpshufbitqmb128_mask:
   case X86::BI__builtin_ia32_vpshufbitqmb256_mask:
   case X86::BI__builtin_ia32_vpshufbitqmb512_mask:
diff --git a/clang/test/CIR/CodeGen/X86/avx512vbmi-builtins.c b/clang/test/CIR/CodeGen/X86/avx512vbmi-builtins.c
new file mode 100644
index 0000000000000..e5f7865af162e
--- /dev/null
+++ b/clang/test/CIR/CodeGen/X86/avx512vbmi-builtins.c
@@ -0,0 +1,22 @@
+// RUN: %clang_cc1 -triple x86_64-unknown-linux-gnu -target-feature +avx512vbmi \
+// RUN:   -fclangir -emit-cir %s -o - | FileCheck %s
+
+#include <immintrin.h>
+__m512i test_multishift(__m512i x, __m512i y) {
+  return _mm512_multishift_epi64_epi8(x, y);
+}
+
+// // CHECK: cir.func @test_multishift
+// // CHECK: cir.call @__builtin_ia32_vpmultishiftqb512
+
+__m128i test_mm_multishift_epi64_epi8(__m128i __X, __m128i __Y)
+{
+  return (__m128i)_mm_multishift_epi64_epi8((__v16qi)__X, (__v16qi)__Y);
+}
+
+
+
+__m256i test_mm256_multishift_epi64_epi8(__m256i __X, __m256i __Y)
+{
+  return (__m256i)_mm256_multishift_epi64_epi8((__v32qi)__X, (__v32qi)__Y);
+}
\ No newline at end of file