Coverage for src/flag_gems/ops/addcdiv.py: 94%

1import logging 

2 

3import torch 

4import triton 

5 

6from flag_gems.utils import pointwise_dynamic 

7 

8logger = logging.getLogger(__name__) 

9 

10 

11@pointwise_dynamic( 

12 is_tensor=[True, True, True, False], promotion_methods=[(0, 1, 2, "DEFAULT")] 

13) 

14@triton.jit 

15def addcdiv_kernel(x, t1, t2, value): 

16 return x + value * (t1 / t2) 

17 

18 

19def addcdiv_out(inp, tensor1, tensor2, *, value=1.0, out): 

20 logger.debug("GEMS ADDCDIV_OUT") 

21 addcdiv_kernel(inp, tensor1, tensor2, value, out0=out) 

22 return out 

23 

24 

25def addcdiv(inp, tensor1, tensor2, value=1.0): 

26 """Functional entry; CUDA may dispatch here without hitting ``addcdiv.out``.""" 

27 logger.debug("GEMS ADDCDIV") 

28 out = torch.empty_like(inp) 

29 return addcdiv_kernel(inp, tensor1, tensor2, value, out0=out)