Skip to content

Commit 113e62c

Browse files
RiverDaveRiverDave
authored
[CIR][CIRGen][Builtin][X86] Lower avx512 gather intrinsics (#1785)
1 parent 6ca3828 commit 113e62c

File tree

3 files changed

+368
-4
lines changed

3 files changed

+368
-4
lines changed

‎clang/lib/CIR/CodeGen/CIRGenBuiltinX86.cpp‎

Lines changed: 89 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -725,8 +725,95 @@ mlir::Value CIRGenFunction::emitX86BuiltinExpr(unsigned BuiltinID,
725725
case X86::BI__builtin_ia32_gathersiv8di:
726726
case X86::BI__builtin_ia32_gathersiv16si:
727727
case X86::BI__builtin_ia32_gatherdiv8di:
728-
case X86::BI__builtin_ia32_gatherdiv16si:
729-
llvm_unreachable("gather3div2df NYI");
728+
case X86::BI__builtin_ia32_gatherdiv16si: {
729+
StringRef intrinsicName;
730+
switch (BuiltinID) {
731+
default:
732+
llvm_unreachable("Unexpected builtin");
733+
case X86::BI__builtin_ia32_gather3div2df:
734+
intrinsicName = "x86.avx512.mask.gather3div2.df";
735+
break;
736+
case X86::BI__builtin_ia32_gather3div2di:
737+
intrinsicName = "x86.avx512.mask.gather3div2.di";
738+
break;
739+
case X86::BI__builtin_ia32_gather3div4df:
740+
intrinsicName = "x86.avx512.mask.gather3div4.df";
741+
break;
742+
case X86::BI__builtin_ia32_gather3div4di:
743+
intrinsicName = "x86.avx512.mask.gather3div4.di";
744+
break;
745+
case X86::BI__builtin_ia32_gather3div4sf:
746+
intrinsicName = "x86.avx512.mask.gather3div4.sf";
747+
break;
748+
case X86::BI__builtin_ia32_gather3div4si:
749+
intrinsicName = "x86.avx512.mask.gather3div4.si";
750+
break;
751+
case X86::BI__builtin_ia32_gather3div8sf:
752+
intrinsicName = "x86.avx512.mask.gather3div8.sf";
753+
break;
754+
case X86::BI__builtin_ia32_gather3div8si:
755+
intrinsicName = "x86.avx512.mask.gather3div8.si";
756+
break;
757+
case X86::BI__builtin_ia32_gather3siv2df:
758+
intrinsicName = "x86.avx512.mask.gather3siv2.df";
759+
break;
760+
case X86::BI__builtin_ia32_gather3siv2di:
761+
intrinsicName = "x86.avx512.mask.gather3siv2.di";
762+
break;
763+
case X86::BI__builtin_ia32_gather3siv4df:
764+
intrinsicName = "x86.avx512.mask.gather3siv4.df";
765+
break;
766+
case X86::BI__builtin_ia32_gather3siv4di:
767+
intrinsicName = "x86.avx512.mask.gather3siv4.di";
768+
break;
769+
case X86::BI__builtin_ia32_gather3siv4sf:
770+
intrinsicName = "x86.avx512.mask.gather3siv4.sf";
771+
break;
772+
case X86::BI__builtin_ia32_gather3siv4si:
773+
intrinsicName = "x86.avx512.mask.gather3siv4.si";
774+
break;
775+
case X86::BI__builtin_ia32_gather3siv8sf:
776+
intrinsicName = "x86.avx512.mask.gather3siv8.sf";
777+
break;
778+
case X86::BI__builtin_ia32_gather3siv8si:
779+
intrinsicName = "x86.avx512.mask.gather3siv8.si";
780+
break;
781+
case X86::BI__builtin_ia32_gathersiv8df:
782+
intrinsicName = "x86.avx512.mask.gather.dpd.512";
783+
break;
784+
case X86::BI__builtin_ia32_gathersiv16sf:
785+
intrinsicName = "x86.avx512.mask.gather.dps.512";
786+
break;
787+
case X86::BI__builtin_ia32_gatherdiv8df:
788+
intrinsicName = "x86.avx512.mask.gather.qpd.512";
789+
break;
790+
case X86::BI__builtin_ia32_gatherdiv16sf:
791+
intrinsicName = "x86.avx512.mask.gather.qps.512";
792+
break;
793+
case X86::BI__builtin_ia32_gathersiv8di:
794+
intrinsicName = "x86.avx512.mask.gather.dpq.512";
795+
break;
796+
case X86::BI__builtin_ia32_gathersiv16si:
797+
intrinsicName = "x86.avx512.mask.gather.dpi.512";
798+
break;
799+
case X86::BI__builtin_ia32_gatherdiv8di:
800+
intrinsicName = "x86.avx512.mask.gather.qpq.512";
801+
break;
802+
case X86::BI__builtin_ia32_gatherdiv16si:
803+
intrinsicName = "x86.avx512.mask.gather.qpi.512";
804+
break;
805+
}
806+
807+
unsigned minElts =
808+
std::min(cast<cir::VectorType>(Ops[0].getType()).getSize(),
809+
cast<cir::VectorType>(Ops[2].getType()).getSize());
810+
Ops[3] = getMaskVecValue(*this, Ops[3], minElts, getLoc(E->getExprLoc()));
811+
return builder
812+
.create<cir::LLVMIntrinsicCallOp>(
813+
getLoc(E->getExprLoc()), builder.getStringAttr(intrinsicName.str()),
814+
convertType(E->getType()), Ops)
815+
.getResult();
816+
}
730817
case X86::BI__builtin_ia32_scattersiv8df:
731818
case X86::BI__builtin_ia32_scattersiv16sf:
732819
case X86::BI__builtin_ia32_scatterdiv8df:

‎clang/test/CIR/CodeGen/X86/avx512f-builtins.c‎

Lines changed: 135 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -372,4 +372,138 @@ void test_mm512_mask_compressstoreu_epi32(void *__P, __mmask16 __U, __m512i __A)
372372
// LLVM-LABEL: test_mm512_mask_compressstoreu_epi32
373373
// LLVM: @llvm.masked.compressstore.v16i32(<16 x i32> %{{.*}}, ptr %{{.*}}, <16 x i1> %{{.*}})
374374
return _mm512_mask_compressstoreu_epi32(__P, __U, __A);
375-
}
375+
}
376+
__m512d test_mm512_i32gather_pd(__m256i __index, void const *__addr) {
377+
// CIR-LABEL: _mm512_i32gather_pd
378+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpd.512"
379+
380+
// LLVM-LABEL: test_mm512_i32gather_pd
381+
// LLVM: @llvm.x86.avx512.mask.gather.dpd.512
382+
return _mm512_i32gather_pd(__index, __addr, 2);
383+
}
384+
385+
__m512d test_mm512_mask_i32gather_pd(__m512d __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
386+
// CIR-LABEL: _mm512_mask_i32gather_pd
387+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpd.512"
388+
389+
// LLVM-LABEL: test_mm512_mask_i32gather_pd
390+
// LLVM: @llvm.x86.avx512.mask.gather.dpd.512
391+
return _mm512_mask_i32gather_pd(__v1_old, __mask, __index, __addr, 2);
392+
}
393+
394+
__m512 test_mm512_i32gather_ps(__m512i __index, void const *__addr) {
395+
// CIR-LABEL: _mm512_i32gather_ps
396+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dps.512"
397+
398+
// LLVM-LABEL: test_mm512_i32gather_ps
399+
// LLVM: @llvm.x86.avx512.mask.gather.dps.512
400+
return _mm512_i32gather_ps(__index, __addr, 2);
401+
}
402+
403+
__m512d test_mm512_i64gather_pd(__m512i __index, void const *__addr) {
404+
// CIR-LABEL: _mm512_i64gather_pd
405+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpd.512"
406+
407+
// LLVM-LABEL: test_mm512_i64gather_pd
408+
// CHECK: @llvm.x86.avx512.mask.gather.qpd.512
409+
return _mm512_i64gather_pd(__index, __addr, 2);
410+
}
411+
412+
__m512d test_mm512_mask_i64gather_pd(__m512d __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) {
413+
// CIR-LABEL: _mm512_mask_i64gather_pd
414+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpd.512"
415+
416+
// LLVM-LABEL: test_mm512_mask_i64gather_pd
417+
// CHECK: @llvm.x86.avx512.mask.gather.qpd.512
418+
return _mm512_mask_i64gather_pd(__v1_old, __mask, __index, __addr, 2);
419+
}
420+
421+
__m256 test_mm512_i64gather_ps(__m512i __index, void const *__addr) {
422+
// CIR-LABEL: _mm512_i64gather_ps
423+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qps.512"
424+
425+
// LLVM-LABEL: test_mm512_i64gather_ps
426+
// LLVM: @llvm.x86.avx512.mask.gather.qps.512
427+
return _mm512_i64gather_ps(__index, __addr, 2);
428+
}
429+
430+
__m256 test_mm512_mask_i64gather_ps(__m256 __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) {
431+
// CIR-LABEL: _mm512_mask_i64gather_ps
432+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qps.512"
433+
434+
// LLVM-LABEL: test_mm512_mask_i64gather_ps
435+
// LLVM: @llvm.x86.avx512.mask.gather.qps.512
436+
return _mm512_mask_i64gather_ps(__v1_old, __mask, __index, __addr, 2);
437+
}
438+
439+
__m512i test_mm512_i32gather_epi64(__m256i __index, void const *__addr) {
440+
// CIR-LABEL: _mm512_i32gather_epi64
441+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpq.512"
442+
443+
// LLVM-LABEL: test_mm512_i32gather_epi64
444+
// LLVM: @llvm.x86.avx512.mask.gather.dpq.512
445+
return _mm512_i32gather_epi64(__index, __addr, 2);
446+
}
447+
448+
__m512i test_mm512_mask_i32gather_epi64(__m512i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
449+
// CIR-LABEL: _mm512_mask_i32gather_epi64
450+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpq.512"
451+
452+
// LLVM-LABEL: test_mm512_mask_i32gather_epi64
453+
// LLVM: @llvm.x86.avx512.mask.gather.dpq.512
454+
return _mm512_mask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2);
455+
}
456+
457+
__m512i test_mm512_i32gather_epi32(__m512i __index, void const *__addr) {
458+
// CIR-LABEL: _mm512_i32gather_epi32
459+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpi.512"
460+
461+
// LLVM-LABEL: test_mm512_i32gather_epi32
462+
// LLVM: @llvm.x86.avx512.mask.gather.dpi.512
463+
return _mm512_i32gather_epi32(__index, __addr, 2);
464+
}
465+
466+
__m512i test_mm512_mask_i32gather_epi32(__m512i __v1_old, __mmask16 __mask, __m512i __index, void const *__addr) {
467+
// CIR-LABEL: _mm512_mask_i32gather_epi32
468+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.dpi.512"
469+
470+
// LLVM-LABEL: test_mm512_mask_i32gather_epi32
471+
// LLVM: @llvm.x86.avx512.mask.gather.dpi.512
472+
return _mm512_mask_i32gather_epi32(__v1_old, __mask, __index, __addr, 2);
473+
}
474+
475+
__m512i test_mm512_i64gather_epi64(__m512i __index, void const *__addr) {
476+
// CIR-LABEL: _mm512_i64gather_epi64
477+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpq.512"
478+
479+
// LLVM-LABEL: test_mm512_i64gather_epi64
480+
// LLVM: @llvm.x86.avx512.mask.gather.qpq.512
481+
return _mm512_i64gather_epi64(__index, __addr, 2);
482+
}
483+
484+
__m512i test_mm512_mask_i64gather_epi64(__m512i __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) {
485+
// CIR-LABEL: _mm512_mask_i64gather_epi64
486+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpq.512"
487+
488+
// LLVM-LABEL: test_mm512_mask_i64gather_epi64
489+
// LLVM: @llvm.x86.avx512.mask.gather.qpq.512
490+
return _mm512_mask_i64gather_epi64(__v1_old, __mask, __index, __addr, 2);
491+
}
492+
493+
__m256i test_mm512_i64gather_epi32(__m512i __index, void const *__addr) {
494+
// CIR-LABEL: _mm512_i64gather_epi32
495+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpi.512"
496+
497+
// LLVM-LABEL: test_mm512_i64gather_epi32
498+
// LLVM: @llvm.x86.avx512.mask.gather.qpi.512
499+
return _mm512_i64gather_epi32(__index, __addr, 2);
500+
}
501+
502+
__m256i test_mm512_mask_i64gather_epi32(__m256i __v1_old, __mmask8 __mask, __m512i __index, void const *__addr) {
503+
// CIR-LABEL: _mm512_mask_i64gather_epi32
504+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather.qpi.512"
505+
506+
// LLVM-LABEL: test_mm512_mask_i64gather_epi32
507+
// LLVM: @llvm.x86.avx512.mask.gather.qpi.512
508+
return _mm512_mask_i64gather_epi32(__v1_old, __mask, __index, __addr, 2);
509+
}

‎clang/test/CIR/CodeGen/X86/avx512vl-builtins.c‎

Lines changed: 144 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -597,4 +597,147 @@ void test_mm256_mask_compressstoreu_epi32(void *__P, __mmask8 __U, __m256i __A)
597597
// LLVM-LABEL: @test_mm256_mask_compressstoreu_epi32
598598
// LLVM: @llvm.masked.compressstore.v8i32(<8 x i32> %{{.*}}, ptr %{{.*}}, <8 x i1> %{{.*}})
599599
return _mm256_mask_compressstoreu_epi32(__P,__U,__A);
600-
}
600+
}
601+
__m128d test_mm_mmask_i64gather_pd(__m128d __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
602+
// CIR-LABEL: test_mm_mmask_i64gather_pd
603+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div2.df"
604+
605+
// LLVM-LABEL: @test_mm_mmask_i64gather_pd
606+
// LLVM: @llvm.x86.avx512.mask.gather3div2.df
607+
return _mm_mmask_i64gather_pd(__v1_old, __mask, __index, __addr, 2);
608+
}
609+
610+
__m128i test_mm_mmask_i64gather_epi64(__m128i __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
611+
// CIR-LABEL: test_mm_mmask_i64gather_epi64
612+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div2.di"
613+
614+
// LLVM-LABEL: @test_mm_mmask_i64gather_epi64
615+
// LLVM: @llvm.x86.avx512.mask.gather3div2.di
616+
return _mm_mmask_i64gather_epi64(__v1_old, __mask, __index, __addr, 2);
617+
}
618+
619+
__m256d test_mm256_mmask_i64gather_pd(__m256d __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
620+
// CIR-LABEL: test_mm256_mmask_i64gather_pd
621+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div4.df"
622+
623+
// LLVM-LABEL: @test_mm256_mmask_i64gather_pd
624+
// LLVM: @llvm.x86.avx512.mask.gather3div4.df
625+
return _mm256_mmask_i64gather_pd(__v1_old, __mask, __index, __addr, 2);
626+
}
627+
628+
__m256i test_mm256_mmask_i64gather_epi64(__m256i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
629+
// CIR-LABEL: test_mm256_mmask_i64gather_epi64
630+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div4.di"
631+
632+
// LLVM-LABEL: @test_mm256_mmask_i64gather_epi64
633+
// LLVM: @llvm.x86.avx512.mask.gather3div4.di
634+
return _mm256_mmask_i64gather_epi64(__v1_old, __mask, __index, __addr, 2);
635+
}
636+
637+
__m128 test_mm_mmask_i64gather_ps(__m128 __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
638+
// CIR-LABEL: test_mm_mmask_i64gather_ps
639+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div4.sf"
640+
641+
// LLVM-LABEL: @test_mm_mmask_i64gather_ps
642+
// LLVM: @llvm.x86.avx512.mask.gather3div4.sf
643+
return _mm_mmask_i64gather_ps(__v1_old, __mask, __index, __addr, 2);
644+
}
645+
646+
__m128i test_mm_mmask_i64gather_epi32(__m128i __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
647+
// CIR-LABEL: test_mm_mmask_i64gather_epi32
648+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div4.si"
649+
650+
// LLVM-LABEL: @test_mm_mmask_i64gather_epi32
651+
// LLVM: @llvm.x86.avx512.mask.gather3div4.si
652+
return _mm_mmask_i64gather_epi32(__v1_old, __mask, __index, __addr, 2);
653+
}
654+
655+
__m128 test_mm256_mmask_i64gather_ps(__m128 __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
656+
// CIR-LABEL: test_mm256_mmask_i64gather_ps
657+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div8.sf"
658+
659+
// LLVM-LABEL: @test_mm256_mmask_i64gather_ps
660+
// LLVM: @llvm.x86.avx512.mask.gather3div8.sf
661+
return _mm256_mmask_i64gather_ps(__v1_old, __mask, __index, __addr, 2);
662+
}
663+
664+
__m128i test_mm256_mmask_i64gather_epi32(__m128i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
665+
// CIR-LABEL: test_mm256_mmask_i64gather_epi32
666+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3div8.si"
667+
668+
// LLVM-LABEL: @test_mm256_mmask_i64gather_epi32
669+
// LLVM: @llvm.x86.avx512.mask.gather3div8.si
670+
return _mm256_mmask_i64gather_epi32(__v1_old, __mask, __index, __addr, 2);
671+
}
672+
673+
__m128d test_mm_mask_i32gather_pd(__m128d __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
674+
// CIR-LABEL: test_mm_mask_i32gather_pd
675+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv2.df"
676+
677+
// LLVM-LABEL: @test_mm_mask_i32gather_pd
678+
// LLVM: @llvm.x86.avx512.mask.gather3siv2.df
679+
return _mm_mmask_i32gather_pd(__v1_old, __mask, __index, __addr, 2);
680+
}
681+
682+
__m128i test_mm_mask_i32gather_epi64(__m128i __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
683+
// CIR-LABEL: test_mm_mask_i32gather_epi64
684+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv2.di"
685+
686+
// LLVM-LABEL: @test_mm_mask_i32gather_epi64
687+
// LLVM: @llvm.x86.avx512.mask.gather3siv2.di
688+
return _mm_mmask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2);
689+
}
690+
691+
__m256d test_mm256_mask_i32gather_pd(__m256d __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
692+
// CIR-LABEL: test_mm256_mask_i32gather_pd
693+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv4.df"
694+
695+
// LLVM-LABEL: @test_mm256_mask_i32gather_pd
696+
// LLVM: @llvm.x86.avx512.mask.gather3siv4.df
697+
return _mm256_mmask_i32gather_pd(__v1_old, __mask, __index, __addr, 2);
698+
}
699+
700+
__m256i test_mm256_mask_i32gather_epi64(__m256i __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
701+
// CIR-LABEL: test_mm256_mask_i32gather_epi64
702+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv4.di"
703+
704+
// LLVM-LABEL: @test_mm256_mask_i32gather_epi64
705+
// LLVM: @llvm.x86.avx512.mask.gather3siv4.di
706+
return _mm256_mmask_i32gather_epi64(__v1_old, __mask, __index, __addr, 2);
707+
}
708+
709+
__m128 test_mm_mask_i32gather_ps(__m128 __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
710+
// CIR-LABEL: test_mm_mask_i32gather_ps
711+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv4.sf"
712+
713+
// LLVM-LABEL: @test_mm_mask_i32gather_ps
714+
// LLVM: @llvm.x86.avx512.mask.gather3siv4.sf
715+
return _mm_mmask_i32gather_ps(__v1_old, __mask, __index, __addr, 2);
716+
}
717+
718+
__m128i test_mm_mask_i32gather_epi32(__m128i __v1_old, __mmask8 __mask, __m128i __index, void const *__addr) {
719+
// CIR-LABEL: test_mm_mask_i32gather_epi32
720+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv4.si"
721+
722+
// LLVM-LABEL: @test_mm_mask_i32gather_epi32
723+
// LLVM: @llvm.x86.avx512.mask.gather3siv4.si
724+
return _mm_mmask_i32gather_epi32(__v1_old, __mask, __index, __addr, 2);
725+
}
726+
727+
__m256 test_mm256_mask_i32gather_ps(__m256 __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
728+
// CIR-LABEL: test_mm256_mask_i32gather_ps
729+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv8.sf"
730+
731+
// LLVM-LABEL: @test_mm256_mask_i32gather_ps
732+
// LLVM: @llvm.x86.avx512.mask.gather3siv8.sf
733+
return _mm256_mmask_i32gather_ps(__v1_old, __mask, __index, __addr, 2);
734+
}
735+
736+
__m256i test_mm256_mask_i32gather_epi32(__m256i __v1_old, __mmask8 __mask, __m256i __index, void const *__addr) {
737+
// CIR-LABEL: test_mm256_mask_i32gather_epi32
738+
// CIR: cir.llvm.intrinsic "x86.avx512.mask.gather3siv8.si"
739+
740+
// LLVM-LABEL: @test_mm256_mask_i32gather_epi32
741+
// LLVM: @llvm.x86.avx512.mask.gather3siv8.si
742+
return _mm256_mmask_i32gather_epi32(__v1_old, __mask, __index, __addr, 2);
743+
}

0 commit comments

Comments
 (0)