Upload 9 files

Trained_20G/config.json

@@ -1,8 +1,11 @@
 {
-  "_name_or_path": "/home/yueyulin/model/qwen_r1_7b_withgate_freezemlp__20G_hf/",
   "architectures": [
     "RwkvHybridForCausalLM"
   ],
+  "auto_map": {
+      "AutoConfig": "configuration_rwkv_hybrid.RwkvHybridConfig",
+      "AutoModelForCausalLM": "modeling_rwkv_hybrid.RwkvHybridForCausalLM"
+  },
   "attention_dropout": 0.0,
   "bos_token_id": 151643,
   "eos_token_id": 151645,

Trained_20G/configuration_rwkv_hybrid.py

@@ -0,0 +1,254 @@
+# coding=utf-8
+# Copyright 2025 RWKV team. All rights reserved.
+# Copyright 2024 The Qwen team, Alibaba Group and the HuggingFace Inc. team. All rights reserved.
+#
+# Licensed under the Apache License, Version 2.0 (the "License");
+# you may not use this file except in compliance with the License.
+# You may obtain a copy of the License at
+#
+#     http://www.apache.org/licenses/LICENSE-2.0
+#
+# Unless required by applicable law or agreed to in writing, software
+# distributed under the License is distributed on an "AS IS" BASIS,
+# WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
+# See the License for the specific language governing permissions and
+# limitations under the License.
+"""RwkvHybrid model configuration"""
+
+from transformers.configuration_utils import PretrainedConfig
+from transformers.modeling_rope_utils import rope_config_validation
+from transformers.utils import logging
+from typing import Optional, Union, List
+
+
+logger = logging.get_logger(__name__)
+
+
+class RwkvHybridConfig(PretrainedConfig):
+    r"""
+    This is the configuration class to store the configuration of a [`RwkvHybridModel`]. It is used to instantiate a
+    RwkvHybrid model according to the specified arguments, defining the model architecture. Instantiating a configuration
+    with the defaults will yield a similar configuration to that of
+    RwkvHybrid-7B-beta.
+
+    Configuration objects inherit from [`PretrainedConfig`] and can be used to control the model outputs. Read the
+    documentation from [`PretrainedConfig`] for more information.
+
+
+    Args:
+        vocab_size (`int`, *optional*, defaults to 151936):
+            Vocabulary size of the RwkvHybrid model. Defines the number of different tokens that can be represented by the
+            `inputs_ids` passed when calling [`RwkvHybridModel`]
+        hidden_size (`int`, *optional*, defaults to 4096):
+            Dimension of the hidden representations.
+        intermediate_size (`int`, *optional*, defaults to 22016):
+            Dimension of the MLP representations.
+        num_hidden_layers (`int`, *optional*, defaults to 32):
+            Number of hidden layers in the Transformer encoder.
+        num_attention_heads (`int`, *optional*, defaults to 32):
+            Number of attention heads for each attention layer in the Transformer encoder.
+        num_key_value_heads (`int`, *optional*, defaults to 32):
+            This is the number of key_value heads that should be used to implement Grouped Query Attention. If
+            `num_key_value_heads=num_attention_heads`, the model will use Multi Head Attention (MHA), if
+            `num_key_value_heads=1` the model will use Multi Query Attention (MQA) otherwise GQA is used. When
+            converting a multi-head checkpoint to a GQA checkpoint, each group key and value head should be constructed
+            by meanpooling all the original heads within that group. For more details checkout [this
+            paper](https://arxiv.org/pdf/2305.13245.pdf). If it is not specified, will default to `32`.
+        hidden_act (`str` or `function`, *optional*, defaults to `"silu"`):
+            The non-linear activation function (function or string) in the decoder.
+        max_position_embeddings (`int`, *optional*, defaults to 32768):
+            The maximum sequence length that this model might ever be used with.
+        initializer_range (`float`, *optional*, defaults to 0.02):
+            The standard deviation of the truncated_normal_initializer for initializing all weight matrices.
+        rms_norm_eps (`float`, *optional*, defaults to 1e-06):
+            The epsilon used by the rms normalization layers.
+        use_cache (`bool`, *optional*, defaults to `True`):
+            Whether or not the model should return the last key/values attentions (not used by all models). Only
+            relevant if `config.is_decoder=True`.
+        tie_word_embeddings (`bool`, *optional*, defaults to `False`):
+            Whether the model's input and output word embeddings should be tied.
+        rope_theta (`float`, *optional*, defaults to 10000.0):
+            The base period of the RoPE embeddings.
+        rope_scaling (`Dict`, *optional*):
+            Dictionary containing the scaling configuration for the RoPE embeddings. NOTE: if you apply new rope type
+            and you expect the model to work on longer `max_position_embeddings`, we recommend you to update this value
+            accordingly.
+            Expected contents:
+                `rope_type` (`str`):
+                    The sub-variant of RoPE to use. Can be one of ['default', 'linear', 'dynamic', 'yarn', 'longrope',
+                    'llama3'], with 'default' being the original RoPE implementation.
+                `factor` (`float`, *optional*):
+                    Used with all rope types except 'default'. The scaling factor to apply to the RoPE embeddings. In
+                    most scaling types, a `factor` of x will enable the model to handle sequences of length x *
+                    original maximum pre-trained length.
+                `original_max_position_embeddings` (`int`, *optional*):
+                    Used with 'dynamic', 'longrope' and 'llama3'. The original max position embeddings used during
+                    pretraining.
+                `attention_factor` (`float`, *optional*):
+                    Used with 'yarn' and 'longrope'. The scaling factor to be applied on the attention
+                    computation. If unspecified, it defaults to value recommended by the implementation, using the
+                    `factor` field to infer the suggested value.
+                `beta_fast` (`float`, *optional*):
+                    Only used with 'yarn'. Parameter to set the boundary for extrapolation (only) in the linear
+                    ramp function. If unspecified, it defaults to 32.
+                `beta_slow` (`float`, *optional*):
+                    Only used with 'yarn'. Parameter to set the boundary for interpolation (only) in the linear
+                    ramp function. If unspecified, it defaults to 1.
+                `short_factor` (`List[float]`, *optional*):
+                    Only used with 'longrope'. The scaling factor to be applied to short contexts (<
+                    `original_max_position_embeddings`). Must be a list of numbers with the same length as the hidden
+                    size divided by the number of attention heads divided by 2
+                `long_factor` (`List[float]`, *optional*):
+                    Only used with 'longrope'. The scaling factor to be applied to long contexts (<
+                    `original_max_position_embeddings`). Must be a list of numbers with the same length as the hidden
+                    size divided by the number of attention heads divided by 2
+                `low_freq_factor` (`float`, *optional*):
+                    Only used with 'llama3'. Scaling factor applied to low frequency components of the RoPE
+                `high_freq_factor` (`float`, *optional*):
+                    Only used with 'llama3'. Scaling factor applied to high frequency components of the RoPE
+        use_sliding_window (`bool`, *optional*, defaults to `False`):
+            Whether to use sliding window attention.
+        sliding_window (`int`, *optional*, defaults to 4096):
+            Sliding window attention (SWA) window size. If not specified, will default to `4096`.
+        max_window_layers (`int`, *optional*, defaults to 28):
+            The number of layers that use SWA (Sliding Window Attention). The bottom layers use SWA while the top use full attention.
+        attention_dropout (`float`, *optional*, defaults to 0.0):
+            The dropout ratio for the attention probabilities.
+        head_size (`int`, *optional*, defaults to 64):
+            Dimensionality of each RWKV attention head. Defines the hidden dimension size for RWKV attention mechanisms.
+        head_size_divisor (`int`, *optional*, defaults to 8):
+            Constraint for head_size initialization, typically set to the square root of head_size. Ensures divisibility
+            between hidden_size and head_size.
+        wkv_version (`int`, *optional*, defaults to 7):
+            Version of RWKV attention implementation. Currently supports:
+            - 6: Original implementation requiring `wkv_has_gate=True` and `wkv_use_vfirst=False`
+            - 7: Improved version requiring `wkv_use_vfirst=True`
+        wkv_has_gate (`bool`, *optional*, defaults to False):
+            Whether to include gating mechanism in RWKV attention. Required for version 6.
+        wkv_has_group_norm (`bool`, *optional*, defaults to True):
+            Whether to apply group normalization in RWKV attention layers.
+        wkv_use_vfirst (`bool`, *optional*, defaults to True):
+            Whether to prioritize value projection in RWKV attention computation. Required for version 7.
+        wkv_layers (`Union[str, List[int]]`, *optional*, defaults to None):
+            Specifies which layers use RWKV attention:
+            - `"full"` or `None`: All layers use RWKV
+            - List of integers: Only specified layers (e.g., `[0,1,2]`) use RWKV attention
+
+    ```python
+    >>> from transformers import RwkvHybridModel, RwkvHybridConfig
+
+    >>> # Initializing a RwkvHybrid style configuration
+    >>> configuration = RwkvHybridConfig()
+
+    >>> # Initializing a model from the RwkvHybrid-7B style configuration
+    >>> model = RwkvHybridModel(configuration)
+
+    >>> # Accessing the model configuration
+    >>> configuration = model.config
+    ```"""
+
+    model_type = "rwkv_hybrid"
+    keys_to_ignore_at_inference = ["past_key_values"]
+
+    # Default tensor parallel plan for base model `RwkvHybrid`
+    base_model_tp_plan = {
+        "layers.*.self_attn.q_proj": "colwise",
+        "layers.*.self_attn.k_proj": "colwise",
+        "layers.*.self_attn.v_proj": "colwise",
+        "layers.*.self_attn.o_proj": "rowwise",
+        "layers.*.mlp.gate_proj": "colwise",
+        "layers.*.mlp.up_proj": "colwise",
+        "layers.*.mlp.down_proj": "rowwise",
+    }
+
+    def __init__(
+        self,
+        vocab_size: int = 151936,
+        hidden_size: int = 4096,
+        intermediate_size: int = 22016,
+        num_hidden_layers: int = 32,
+        num_attention_heads: int = 32,
+        num_key_value_heads: int = 32,
+        head_size: int = 64,
+        head_size_divisor: int = 8,
+        hidden_act: str = "silu",
+        max_position_embeddings: int = 32768,
+        initializer_range: float = 0.02,
+        rms_norm_eps: float = 1e-6,
+        use_cache: bool = True,
+        tie_word_embeddings: bool = False,
+        rope_theta: float = 10000.0,
+        rope_scaling: Optional[dict] = None,
+        use_sliding_window: bool = False,
+        sliding_window: int = 4096,
+        max_window_layers: int = 28,
+        attention_dropout: float = 0.0,
+        wkv_version: int = 7,
+        wkv_has_gate: bool = False,
+        wkv_has_group_norm: bool = True,
+        wkv_use_vfirst: bool = True,
+        wkv_layers: Optional[Union[str, List[int]]] = None,
+        **kwargs,
+    ):
+        self.vocab_size = vocab_size
+        self.max_position_embeddings = max_position_embeddings
+        self.hidden_size = hidden_size
+        self.intermediate_size = intermediate_size
+        self.num_hidden_layers = num_hidden_layers
+        self.num_wkv_heads = hidden_size // head_size
+        assert hidden_size % head_size == 0, "hidden_size must be divisible by head_size"
+        self.num_attention_heads = num_attention_heads
+        self.use_sliding_window = use_sliding_window
+        self.sliding_window = sliding_window if use_sliding_window else None
+        self.max_window_layers = max_window_layers
+        self.head_size = head_size
+        self.head_size_divisor = head_size_divisor
+        self.wkv_version = wkv_version
+
+        self.wkv_has_gate = wkv_has_gate
+        self.wkv_has_group_norm = wkv_has_group_norm
+        self.wkv_use_vfirst = wkv_use_vfirst
+
+        if self.wkv_version == 7:
+            assert self.wkv_use_vfirst, "wkv_use_vfirst must be True for wkv_version 7"
+        elif self.wkv_version == 6:
+            assert self.wkv_has_gate, "wkv_has_gate must be True for wkv_version 6"
+            assert not self.wkv_use_vfirst, "wkv_use_vfirst must be False for wkv_version 6"
+        else:
+            raise NotImplementedError(f"Unsupported wkv_version: {self.wkv_version}, \
+                                        wkv_version must be 6 or 7")
+
+        if wkv_layers == "full" or wkv_layers is None:
+            self.wkv_layers = list(range(num_hidden_layers))
+        elif isinstance(wkv_layers, list):
+            if all(isinstance(layer, int) for layer in wkv_layers):
+                self.wkv_layers = wkv_layers
+            else:
+                raise ValueError(
+                    "All elements in wkv_layers must be integers.")
+        else:
+            raise TypeError(
+                "wkv_layers must be either 'full', None, or a list of integers.")
+
+        # for backward compatibility
+        if num_key_value_heads is None:
+            num_key_value_heads = num_attention_heads
+
+        self.num_key_value_heads = num_key_value_heads
+        self.hidden_act = hidden_act
+        self.initializer_range = initializer_range
+        self.rms_norm_eps = rms_norm_eps
+        self.use_cache = use_cache
+        self.rope_theta = rope_theta
+        self.rope_scaling = rope_scaling
+        self.attention_dropout = attention_dropout
+        # Validate the correctness of rotary position embeddings parameters
+        # BC: if there is a 'type' field, move it to 'rope_type'.
+        if self.rope_scaling is not None and "type" in self.rope_scaling:
+            self.rope_scaling["rope_type"] = self.rope_scaling["type"]
+        rope_config_validation(self)
+
+        super().__init__(
+            tie_word_embeddings=tie_word_embeddings,
+            **kwargs,
+        )

Trained_20G/hybrid_cache.py

@@ -0,0 +1,75 @@
+import torch
+from typing import Any, Dict, Optional, Union
+from transformers.cache_utils import DynamicCache
+
+
+class AttnState:
+    def __init__(self, shift_state: torch.Tensor, wkv_state: torch.Tensor):
+        self.shift_state = shift_state
+        self.wkv_state = wkv_state
+
+
+class FfnState:
+    def __init__(self, shift_state: torch.Tensor):
+        self.shift_state = shift_state
+
+
+class BlockState:
+    def __init__(
+        self, 
+        attn_state: AttnState,
+        ffn_state: FfnState
+    ):
+        self.attn_state = attn_state
+        self.ffn_state = ffn_state
+
+class HybridCache(DynamicCache):
+    def __init__(self) -> None:
+        super().__init__()
+        self.rwkv_layers = set()
+        self.key_cache_nums = 0
+        self.v_first_cache = None
+
+    def update(
+        self,
+        key_states: Union[int, torch.Tensor],
+        value_states: Union[torch.Tensor, BlockState],
+        layer_idx: int,
+        cache_kwargs: Optional[Dict[str, Any]] = None
+    ):
+        if isinstance(key_states, int) and isinstance(value_states, BlockState):
+            self.rwkv_layers.add(layer_idx)
+
+            if layer_idx >= self.key_cache_nums:
+                self.key_cache.append([])
+                self.value_cache.append([])
+                self.key_cache[layer_idx].append(key_states)
+                self.value_cache[layer_idx].append(value_states)
+                self.key_cache_nums += 1
+
+            else:
+                self.key_cache[layer_idx][0] += key_states
+                self.value_cache[layer_idx][0] = value_states
+
+            return key_states, value_states
+
+        return super().update(key_states, value_states, layer_idx, cache_kwargs)
+
+    def update_v_first(self, v_first: torch.Tensor):
+        self.v_first_cache = v_first
+
+    def get_v_first(self):
+        return self.v_first_cache
+
+    def get_seq_length(self, layer_idx: Optional[int] = 0):
+        if layer_idx in self.rwkv_layers:
+            return self.key_cache[layer_idx][0]
+        return super().get_seq_length(layer_idx)
+
+    def reorder_cache(self, beam_idx):
+        return super().reorder_cache(beam_idx)
+
+    def __getitem__(self, item):
+        if item in self.rwkv_layers:
+            return self.value_cache[item]
+        return super().__getitem__(item)

Trained_20G/modeling_rwkv_hybrid.py

@@ -0,0 +1,716 @@
+from typing import Callable, List, Optional, Tuple, Union
+
+import torch
+import torch.nn as nn
+from transformers.cache_utils import Cache
+
+from transformers.activations import ACT2FN
+from transformers.cache_utils import Cache, StaticCache
+from .hybrid_cache import HybridCache
+from transformers.generation import GenerationMixin
+from transformers.modeling_attn_mask_utils import AttentionMaskConverter
+from transformers.modeling_flash_attention_utils import FlashAttentionKwargs
+from transformers.modeling_utils import ALL_ATTENTION_FUNCTIONS, PreTrainedModel
+
+from transformers.modeling_outputs import (
+    BaseModelOutputWithPast,
+    CausalLMOutputWithPast,
+)
+from transformers.processing_utils import Unpack
+from transformers.utils import (
+    LossKwargs,
+    add_start_docstrings,
+    add_start_docstrings_to_model_forward,
+    logging,
+)
+
+import threading
+from .wkv import Rwkv7Attention, Rwkv6Attention
+from .configuration_rwkv_hybrid import RwkvHybridConfig
+
+from transformers.models.qwen2.modeling_qwen2 import (Qwen2MLP, 
+                                    Qwen2RMSNorm, 
+                                    Qwen2RotaryEmbedding, 
+                                    Qwen2Attention)
+
+logger = logging.get_logger(__name__)
+
+_CONFIG_FOR_DOC = "RwkvHybridConfig"
+
+
+class RwkvHybridDecoderLayer(nn.Module):
+    def __init__(self, config: RwkvHybridConfig, layer_idx: int):
+        super().__init__()
+        self.hidden_size = config.hidden_size
+
+        self.is_rwkv = True if layer_idx in config.wkv_layers else False
+        if self.is_rwkv:
+            if config.wkv_version == 7:
+                self.self_attn = Rwkv7Attention(
+                    args=config, layer_id=layer_idx)
+            elif config.wkv_version == 6:
+                self.self_attn = Rwkv6Attention(
+                    args=config, layer_id=layer_idx)
+            else:
+                raise NotImplementedError
+        else:
+            self.self_attn = Qwen2Attention(config=config, layer_idx=layer_idx)
+
+        self.mlp = Qwen2MLP(config)
+        self.input_layernorm = Qwen2RMSNorm(
+            config.hidden_size, eps=config.rms_norm_eps)
+        self.post_attention_layernorm = Qwen2RMSNorm(
+            config.hidden_size, eps=config.rms_norm_eps)
+        self.layer_idx = layer_idx
+
+    def forward(
+        self,
+        hidden_states: torch.Tensor,
+        attention_mask: Optional[torch.Tensor] = None,
+        position_ids: Optional[torch.Tensor] = None,
+        past_key_value: Optional[Cache] = None,
+        output_attentions: Optional[bool] = False,
+        use_cache: Optional[bool] = False,
+        cache_position: Optional[torch.Tensor] = None,
+        position_embeddings: Optional[torch.Tensor] = None,
+        sequence_mask: Optional[torch.Tensor] = None,
+        cu_seq_lens_q: Optional[torch.LongTensor] = None,
+        cu_seq_lens_k: Optional[torch.LongTensor] = None,
+        max_length_q: Optional[int] = None,
+        max_length_k: Optional[int] = None,
+        cu_seqlens: Optional[torch.LongTensor] = None,
+        v_first: Optional[torch.LongTensor] = None,
+        **kwargs,
+    ) -> Tuple[torch.FloatTensor, Optional[Tuple[torch.FloatTensor, torch.FloatTensor]]]:
+
+        if sequence_mask is not None:
+            assert len(sequence_mask.shape) == 2, (
+                "Expected attention_mask as a 0-1 matrix with shape [batch_size, seq_len] "
+                "for padding purposes (0 indicating padding). "
+                "Arbitrary attention masks of shape [batch_size, seq_len, seq_len] are not allowed."
+            )
+            hidden_states = hidden_states.mul(
+                sequence_mask[:, -hidden_states.shape[-2]:, None])
+
+        residual = hidden_states
+
+        hidden_states = self.input_layernorm(hidden_states)
+
+        # RWKV attention
+        if self.is_rwkv:
+            hidden_states, self_attn_weights, v_first = self.self_attn(
+                hidden_states=hidden_states,
+                position_ids=position_ids,
+                past_key_value=past_key_value,
+                output_attentions=output_attentions,
+                use_cache=use_cache,
+                cache_position=cache_position,
+                position_embeddings=position_embeddings,
+                cu_seqlens=cu_seqlens,
+                v_first=v_first,
+                **kwargs
+            )
+        else:
+            hidden_states, self_attn_weights = self.self_attn(
+                hidden_states=hidden_states,
+                attention_mask=attention_mask,
+                position_ids=position_ids,
+                past_key_value=past_key_value,
+                output_attentions=output_attentions,
+                use_cache=use_cache,
+                cache_position=cache_position,
+                position_embeddings=position_embeddings,
+                cu_seq_lens_q=cu_seq_lens_q,
+                cu_seq_lens_k=cu_seq_lens_k,
+                max_length_q=max_length_q,
+                max_length_k=max_length_k,
+                **kwargs
+            )
+        hidden_states = residual + hidden_states
+
+        # Fully Connected
+        residual = hidden_states
+        hidden_states = self.post_attention_layernorm(hidden_states)
+        hidden_states = self.mlp(hidden_states)
+        hidden_states = residual + hidden_states
+
+        outputs = (hidden_states,)
+        if output_attentions:
+            outputs += (self_attn_weights,)
+
+        if self.is_rwkv:
+            outputs += (v_first,)
+
+        return outputs
+
+
+RWKV_HYBRID_START_DOCSTRING = r"""
+    This model inherits from [`PreTrainedModel`]. Check the superclass documentation for the generic methods the
+    library implements for all its model (such as downloading or saving, resizing the input embeddings, pruning heads
+    etc.)
+
+    This model is also a PyTorch [torch.nn.Module](https://pytorch.org/docs/stable/nn.html#torch.nn.Module) subclass.
+    Use it as a regular PyTorch Module and refer to the PyTorch documentation for all matter related to general usage
+    and behavior.
+
+    Parameters:
+        config ([`RwkvHybridConfig`]):
+            Model configuration class with all the parameters of the model. Initializing with a config file does not
+            load the weights associated with the model, only the configuration. Check out the
+            [`~PreTrainedModel.from_pretrained`] method to load the model weights.
+"""
+
+
+@add_start_docstrings(
+    "The bare RWKV Hybrid Model outputting raw hidden-states without any specific head on top.",
+    RWKV_HYBRID_START_DOCSTRING,
+)
+class RwkvHybridPreTrainedModel(PreTrainedModel):
+    config_class = RwkvHybridConfig
+    base_model_prefix = "rwkv_hybrid"
+    supports_gradient_checkpointing = True
+    _no_split_modules = ["RwkvHybridDecoderLayer"]
+    _skip_keys_device_placement = ["past_key_values"]
+
+    def _init_weights(self, module):
+        std = self.config.initializer_range
+        if isinstance(module, nn.Linear):
+            module.weight.data.normal_(mean=0.0, std=std)
+            if module.bias is not None:
+                module.bias.data.zero_()
+        elif isinstance(module, nn.Embedding):
+            module.weight.data.normal_(mean=0.0, std=std)
+            if module.padding_idx is not None:
+                module.weight.data[module.padding_idx].zero_()
+
+
+RWKV_HYBRID_INPUTS_DOCSTRING = r"""
+    Args:
+        input_ids (`torch.LongTensor` of shape `(batch_size, sequence_length)`):
+            Indices of input sequence tokens in the vocabulary. Padding will be ignored by default should you provide
+            it.
+
+            Indices can be obtained using [`AutoTokenizer`]. See [`PreTrainedTokenizer.encode`] and
+            [`PreTrainedTokenizer.__call__`] for details.
+
+            [What are input IDs?](../glossary#input-ids)
+        attention_mask (`torch.Tensor` of shape `(batch_size, sequence_length)`, *optional*):
+            Mask to avoid performing attention on padding token indices. Mask values selected in `[0, 1]`:
+
+            - 1 for tokens that are **not masked**,
+            - 0 for tokens that are **masked**.
+
+            [What are attention masks?](../glossary#attention-mask)
+
+            Indices can be obtained using [`AutoTokenizer`]. See [`PreTrainedTokenizer.encode`] and
+            [`PreTrainedTokenizer.__call__`] for details.
+
+            If `past_key_values` is used, optionally only the last `input_ids` have to be input (see
+            `past_key_values`).
+
+            If you want to change padding behavior, you should read [`modeling_opt._prepare_decoder_attention_mask`]
+            and modify to your needs. See diagram 1 in [the paper](https://arxiv.org/abs/1910.13461) for more
+            information on the default strategy.
+
+            - 1 indicates the head is **not masked**,
+            - 0 indicates the head is **masked**.
+        position_ids (`torch.LongTensor` of shape `(batch_size, sequence_length)`, *optional*):
+            Indices of positions of each input sequence tokens in the position embeddings. Selected in the range `[0,
+            config.n_positions - 1]`.
+
+            [What are position IDs?](../glossary#position-ids)
+        past_key_values (`Cache` or `tuple(tuple(torch.FloatTensor))`, *optional*):
+            Pre-computed hidden-states (key and values in the self-attention blocks and in the cross-attention
+            blocks) that can be used to speed up sequential decoding. This typically consists in the `past_key_values`
+            returned by the model at a previous stage of decoding, when `use_cache=True` or `config.use_cache=True`.
+
+            Two formats are allowed:
+            - a [`~cache_utils.Cache`] instance, see our
+            [kv cache guide](https://huggingface.co/docs/transformers/en/kv_cache);
+            - Tuple of `tuple(torch.FloatTensor)` of length `config.n_layers`, with each tuple having 2 tensors of
+            shape `(batch_size, num_heads, sequence_length, embed_size_per_head)`). This is also known as the legacy
+            cache format.
+
+            The model will output the same cache format that is fed as input. If no `past_key_values` are passed, the
+            legacy cache format will be returned.
+
+            If `past_key_values` are used, the user can optionally input only the last `input_ids` (those that don't
+            have their past key value states given to this model) of shape `(batch_size, 1)` instead of all `input_ids`
+            of shape `(batch_size, sequence_length)`.
+        inputs_embeds (`torch.FloatTensor` of shape `(batch_size, sequence_length, hidden_size)`, *optional*):
+            Optionally, instead of passing `input_ids` you can choose to directly pass an embedded representation. This
+            is useful if you want more control over how to convert `input_ids` indices into associated vectors than the
+            model's internal embedding lookup matrix.
+        use_cache (`bool`, *optional*):
+            If set to `True`, `past_key_values` key value states are returned and can be used to speed up decoding (see
+            `past_key_values`).
+        output_attentions (`bool`, *optional*):
+            Whether or not to return the attentions tensors of all attention layers. See `attentions` under returned
+            tensors for more detail.
+        output_hidden_states (`bool`, *optional*):
+            Whether or not to return the hidden states of all layers. See `hidden_states` under returned tensors for
+            more detail.
+        return_dict (`bool`, *optional*):
+            Whether or not to return a [`~utils.ModelOutput`] instead of a plain tuple.
+        cache_position (`torch.LongTensor` of shape `(sequence_length)`, *optional*):
+            Indices depicting the position of the input sequence tokens in the sequence. Contrarily to `position_ids`,
+            this tensor is not affected by padding. It is used to update the cache in the correct position and to infer
+            the complete sequence length.
+"""
+
+
+@add_start_docstrings(
+    "The bare RWKV Hybrid Model outputting raw hidden-states without any specific head on top.",
+    RWKV_HYBRID_START_DOCSTRING,
+)
+class RwkvHybridModel(RwkvHybridPreTrainedModel):
+    """
+    RWKV and Transformer hybrid decoder consisting of *config.num_hidden_layers* layers. Each layer is a [`RwkvHybridDecoderLayer`]
+
+    Args:
+        config: RwkvHybridConfig
+    """
+
+    def __init__(self, config: RwkvHybridConfig):
+        super().__init__(config)
+        self.padding_idx = config.pad_token_id
+        self.vocab_size = config.vocab_size
+
+        self.embed_tokens = nn.Embedding(
+            config.vocab_size, config.hidden_size, self.padding_idx)
+        self.thread_local = threading.local()
+        self.thread_local.v_first = None
+        self.layers = nn.ModuleList(
+            [RwkvHybridDecoderLayer(config, layer_idx)
+             for layer_idx in range(config.num_hidden_layers)]
+        )
+        self.norm = Qwen2RMSNorm(config.hidden_size, eps=config.rms_norm_eps)
+        self.rotary_emb = Qwen2RotaryEmbedding(config=config)
+        self.gradient_checkpointing = False
+
+        # Initialize weights and apply final processing
+        self.post_init()
+
+    def post_init(self):
+        """
+        A method executed at the end of each Transformer model initialization, to execute code that needs the model's
+        modules properly initialized (such as weight initialization).
+        """
+        self.init_weights()
+        self._backward_compatibility_gradient_checkpointing()
+        # If current model is a base model, attach `base_model_tp_plan` from config
+        if self.base_model is self:
+            self._tp_plan = self.config.base_model_tp_plan
+        from transformers.modeling_utils import _init_weights
+        if _init_weights:
+            for layer in self.layers:
+                layer.self_attn.time_mixer.post_init()
+
+    def get_input_embeddings(self):
+        return self.embed_tokens
+
+    def set_input_embeddings(self, value):
+        self.embed_tokens = value
+
+    def get_v_first(self, layer_idx: int, use_cache: bool, past_key_value: HybridCache):
+        if layer_idx == 0:
+            return None
+
+        if use_cache:
+            return past_key_value.get_v_first()
+        return self.v_first
+
+    @add_start_docstrings_to_model_forward(RWKV_HYBRID_INPUTS_DOCSTRING)
+    def forward(
+        self,
+        input_ids: torch.LongTensor = None,
+        attention_mask: Optional[torch.Tensor] = None,
+        position_ids: Optional[torch.LongTensor] = None,
+        past_key_values: Optional[Cache] = None,
+        inputs_embeds: Optional[torch.FloatTensor] = None,
+        use_cache: Optional[bool] = None,
+        output_attentions: Optional[bool] = None,
+        output_hidden_states: Optional[bool] = None,
+        return_dict: Optional[bool] = None,
+        cache_position: Optional[torch.LongTensor] = None,
+        cu_seq_lens_q: Optional[torch.LongTensor] = None,
+        cu_seq_lens_k: Optional[torch.LongTensor] = None,
+        max_length_q: Optional[int] = None,
+        max_length_k: Optional[int] = None,
+        cu_seqlens: Optional[torch.LongTensor] = None,
+        **kwargs,
+    ) -> Union[Tuple, BaseModelOutputWithPast]:
+        output_attentions = output_attentions if output_attentions is not None else self.config.output_attentions
+        output_hidden_states = (
+            output_hidden_states if output_hidden_states is not None else self.config.output_hidden_states
+        )
+        use_cache = use_cache if use_cache is not None else self.config.use_cache
+        return_dict = return_dict if return_dict is not None else self.config.use_return_dict
+
+        if (input_ids is None) ^ (inputs_embeds is not None):
+            raise ValueError(
+                "You must specify exactly one of input_ids or inputs_embeds")
+
+        if self.gradient_checkpointing and self.training and use_cache:
+            logger.warning_once(
+                "`use_cache=True` is incompatible with gradient checkpointing. Setting `use_cache=False`."
+            )
+            use_cache = False
+
+        if inputs_embeds is None:
+            inputs_embeds = self.embed_tokens(input_ids)
+
+        if use_cache and past_key_values is None:
+            past_key_values = HybridCache()
+
+        if cache_position is None:
+            past_seen_tokens = past_key_values.get_seq_length(
+            ) if past_key_values is not None else 0
+            cache_position = torch.arange(
+                past_seen_tokens, past_seen_tokens + inputs_embeds.shape[1], device=inputs_embeds.device
+            )
+
+        if position_ids is None:
+            position_ids = cache_position.unsqueeze(0)
+
+        causal_mask = self._update_causal_mask(
+            attention_mask, inputs_embeds, cache_position, past_key_values, output_attentions
+        )
+
+        hidden_states = inputs_embeds
+
+        # create position embeddings to be shared across the decoder layers
+        position_embeddings = self.rotary_emb(hidden_states, position_ids)
+
+        # decoder layers
+        all_hidden_states = () if output_hidden_states else None
+        all_self_attns = () if output_attentions else None
+
+        for decoder_layer in self.layers[: self.config.num_hidden_layers]:
+            first_rwkv_layer = True
+            if output_hidden_states:
+                all_hidden_states += (hidden_states,)
+
+            if self.gradient_checkpointing and self.training:
+                layer_outputs = self._gradient_checkpointing_func(
+                    decoder_layer.__call__,
+                    hidden_states,
+                    causal_mask,
+                    position_ids,
+                    past_key_values,
+                    output_attentions,
+                    use_cache,
+                    cache_position,
+                    position_embeddings,
+                    attention_mask,
+                    cu_seq_lens_q,
+                    cu_seq_lens_k,
+                    max_length_q,
+                    max_length_k,
+                    cu_seqlens,
+                    self.get_v_first(decoder_layer.layer_idx,
+                                     use_cache, past_key_values)
+                )
+            else:
+                layer_outputs = decoder_layer(
+                    hidden_states,
+                    attention_mask=causal_mask,
+                    position_ids=position_ids,
+                    past_key_value=past_key_values,
+                    output_attentions=output_attentions,
+                    use_cache=use_cache,
+                    cache_position=cache_position,
+                    position_embeddings=position_embeddings,
+                    sequence_mask=attention_mask,
+                    cu_seq_lens_q=cu_seq_lens_q,
+                    cu_seq_lens_k=cu_seq_lens_k,
+                    max_length_q=max_length_q,
+                    max_length_k=max_length_k,
+                    cu_seqlens=cu_seqlens,
+                    v_first=self.get_v_first(
+                        decoder_layer.layer_idx, use_cache, past_key_values)
+                )
+
+            hidden_states = layer_outputs[0]
+
+            if output_attentions:
+                all_self_attns += (layer_outputs[1],)
+
+            if first_rwkv_layer is True and decoder_layer.is_rwkv:
+                v_first = layer_outputs[-1]
+                if use_cache:
+                    past_key_values.update_v_first(v_first)
+                else:
+                    self.register_buffer('v_first', v_first)
+                first_rwkv_layer = False
+
+        hidden_states = self.norm(hidden_states)
+
+        # add hidden states from the last decoder layer
+        if output_hidden_states:
+            all_hidden_states += (hidden_states,)
+
+        output = BaseModelOutputWithPast(
+            last_hidden_state=hidden_states,
+            past_key_values=past_key_values if use_cache else None,
+            hidden_states=all_hidden_states,
+            attentions=all_self_attns,
+        )
+        return output if return_dict else output.to_tuple()
+
+    def _update_causal_mask(
+        self,
+        attention_mask: torch.Tensor,
+        input_tensor: torch.Tensor,
+        cache_position: torch.Tensor,
+        past_key_values: Cache,
+        output_attentions: bool,
+    ):
+        if self.config._attn_implementation == "flash_attention_2":
+            if attention_mask is not None and (attention_mask == 0.0).any():
+                return attention_mask
+            return None
+
+        # For SDPA, when possible, we will rely on its `is_causal` argument instead of its `attn_mask` argument, in
+        # order to dispatch on Flash Attention 2. This feature is not compatible with static cache, as SDPA will fail
+        # to infer the attention mask.
+        past_seen_tokens = past_key_values.get_seq_length(
+        ) if past_key_values is not None else 0
+        using_static_cache = isinstance(past_key_values, StaticCache)
+
+        # When output attentions is True, sdpa implementation's forward method calls the eager implementation's forward
+        if self.config._attn_implementation == "sdpa" and not using_static_cache and not output_attentions:
+            if AttentionMaskConverter._ignore_causal_mask_sdpa(
+                attention_mask,
+                inputs_embeds=input_tensor,
+                past_key_values_length=past_seen_tokens,
+                is_training=self.training,
+            ):
+                return None
+
+        dtype, device = input_tensor.dtype, input_tensor.device
+        sequence_length = input_tensor.shape[1]
+        if using_static_cache:
+            target_length = past_key_values.get_max_cache_shape()
+        else:
+            target_length = (
+                attention_mask.shape[-1]
+                if isinstance(attention_mask, torch.Tensor)
+                else past_seen_tokens + sequence_length + 1
+            )
+
+        # In case the provided `attention` mask is 2D, we generate a causal mask here (4D).
+        causal_mask = self._prepare_4d_causal_attention_mask_with_cache_position(
+            attention_mask,
+            sequence_length=sequence_length,
+            target_length=target_length,
+            dtype=dtype,
+            device=device,
+            cache_position=cache_position,
+            batch_size=input_tensor.shape[0],
+        )
+
+        if (
+            self.config._attn_implementation == "sdpa"
+            and attention_mask is not None
+            and attention_mask.device.type == "cuda"
+            and not output_attentions
+        ):
+            # Attend to all tokens in fully masked rows in the causal_mask, for example the relevant first rows when
+            # using left padding. This is required by F.scaled_dot_product_attention memory-efficient attention path.
+            # Details: https://github.com/pytorch/pytorch/issues/110213
+            min_dtype = torch.finfo(dtype).min
+            causal_mask = AttentionMaskConverter._unmask_unattended(
+                causal_mask, min_dtype)
+
+        return causal_mask
+
+    @staticmethod
+    def _prepare_4d_causal_attention_mask_with_cache_position(
+        attention_mask: torch.Tensor,
+        sequence_length: int,
+        target_length: int,
+        dtype: torch.dtype,
+        device: torch.device,
+        cache_position: torch.Tensor,
+        batch_size: int,
+        **kwargs,
+    ):
+        """
+        Creates a causal 4D mask of shape `(batch_size, 1, query_length, key_value_length)` from a 2D mask of shape
+        `(batch_size, key_value_length)`, or if the input `attention_mask` is already 4D, do nothing.
+
+        Args:
+            attention_mask (`torch.Tensor`):
+                A 2D attention mask of shape `(batch_size, key_value_length)` or a 4D attention mask of shape
+                `(batch_size, 1, query_length, key_value_length)`.
+            sequence_length (`int`):
+                The sequence length being processed.
+            target_length (`int`):
+                The target length: when generating with static cache, the mask should be as long as the static cache,
+                to account for the 0 padding, the part of the cache that is not filled yet.
+            dtype (`torch.dtype`):
+                The dtype to use for the 4D attention mask.
+            device (`torch.device`):
+                The device to plcae the 4D attention mask on.
+            cache_position (`torch.Tensor`):
+                Indices depicting the position of the input sequence tokens in the sequence.
+            batch_size (`torch.Tensor`):
+                Batch size.
+        """
+        if attention_mask is not None and attention_mask.dim() == 4:
+            # In this case we assume that the mask comes already in inverted form and requires no inversion or slicing.
+            causal_mask = attention_mask
+        else:
+            min_dtype = torch.finfo(dtype).min
+            causal_mask = torch.full(
+                (sequence_length,
+                 target_length), fill_value=min_dtype, dtype=dtype, device=device
+            )
+            if sequence_length != 1:
+                causal_mask = torch.triu(causal_mask, diagonal=1)
+            causal_mask *= torch.arange(target_length,
+                                        device=device) > cache_position.reshape(-1, 1)
+            causal_mask = causal_mask[None, None,
+                                      :, :].expand(batch_size, 1, -1, -1)
+            if attention_mask is not None:
+                causal_mask = causal_mask.clone()  # copy to contiguous memory for in-place edit
+                mask_length = attention_mask.shape[-1]
+                padding_mask = causal_mask[:, :, :,
+                                           :mask_length] + attention_mask[:, None, None, :]
+                padding_mask = padding_mask == 0
+                causal_mask[:, :, :, :mask_length] = causal_mask[:, :, :, :mask_length].masked_fill(
+                    padding_mask, min_dtype
+                )
+
+        return causal_mask
+
+
+class KwargsForCausalLM(FlashAttentionKwargs, LossKwargs):
+    ...
+
+
+class RwkvHybridForCausalLM(RwkvHybridPreTrainedModel, GenerationMixin):
+    _tied_weights_keys = ["lm_head.weight"]
+    _tp_plan = {"lm_head": "colwise_rep"}
+
+    def __init__(self, config):
+        super().__init__(config)
+        self.model = RwkvHybridModel(config)
+        self.vocab_size = config.vocab_size
+        self.lm_head = nn.Linear(
+            config.hidden_size, config.vocab_size, bias=False)
+
+        # Initialize weights and apply final processing
+        self.post_init()
+
+    def get_input_embeddings(self):
+        return self.model.embed_tokens
+
+    def set_input_embeddings(self, value):
+        self.model.embed_tokens = value
+
+    def get_output_embeddings(self):
+        return self.lm_head
+
+    def set_output_embeddings(self, new_embeddings):
+        self.lm_head = new_embeddings
+
+    def set_decoder(self, decoder):
+        self.model = decoder
+
+    def get_decoder(self):
+        return self.model
+
+    # @add_start_docstrings_to_model_forward(QWEN2_INPUTS_DOCSTRING)
+    # @replace_return_docstrings(output_type=CausalLMOutputWithPast, config_class=_CONFIG_FOR_DOC)
+    def forward(
+        self,
+        input_ids: torch.LongTensor = None,
+        attention_mask: Optional[torch.Tensor] = None,
+        position_ids: Optional[torch.LongTensor] = None,
+        past_key_values: Optional[Union[Cache,
+                                        List[torch.FloatTensor]]] = None,
+        inputs_embeds: Optional[torch.FloatTensor] = None,
+        labels: Optional[torch.LongTensor] = None,
+        use_cache: Optional[bool] = None,
+        output_attentions: Optional[bool] = None,
+        output_hidden_states: Optional[bool] = None,
+        return_dict: Optional[bool] = None,
+        cache_position: Optional[torch.LongTensor] = None,
+        num_logits_to_keep: int = 0,
+        **kwargs: Unpack[KwargsForCausalLM],
+    ) -> Union[Tuple, CausalLMOutputWithPast]:
+        r"""
+        Args:
+            labels (`torch.LongTensor` of shape `(batch_size, sequence_length)`, *optional*):
+                Labels for computing the masked language modeling loss. Indices should either be in `[0, ...,
+                config.vocab_size]` or -100 (see `input_ids` docstring). Tokens with indices set to `-100` are ignored
+                (masked), the loss is only computed for the tokens with labels in `[0, ..., config.vocab_size]`.
+
+            num_logits_to_keep (`int`, *optional*):
+                Calculate logits for the last `num_logits_to_keep` tokens. If `0`, calculate logits for all
+                `input_ids` (special case). Only last token logits are needed for generation, and calculating them only for that
+                token can save memory, which becomes pretty significant for long sequences or large vocabulary size.
+
+        Returns:
+
+        Example:
+
+        ```python
+        >>> from transformers import AutoTokenizer, RwkvHybridForCausalLM
+
+        >>> model = Qwen2ForCausalLM.from_pretrained("RWKV-Red-Team/ARWKV-7B-Preview-0.1")
+        >>> tokenizer = AutoTokenizer.from_pretrained("RWKV-Red-Team/ARWKV-7B-Preview-0.1")
+
+        >>> prompt = "Hey, are you conscious? Can you talk to me?"
+        >>> inputs = tokenizer(prompt, return_tensors="pt")
+
+        >>> # Generate
+        >>> generate_ids = model.generate(inputs.input_ids, max_length=30)
+        >>> tokenizer.batch_decode(generate_ids, skip_special_tokens=True, clean_up_tokenization_spaces=False)[0]
+        "Hey, are you conscious? Can you talk to me?\nI'm not conscious, but I can talk to you."
+        ```"""
+        output_attentions = output_attentions if output_attentions is not None else self.config.output_attentions
+        output_hidden_states = (
+            output_hidden_states if output_hidden_states is not None else self.config.output_hidden_states
+        )
+        return_dict = return_dict if return_dict is not None else self.config.use_return_dict
+
+        # decoder outputs consists of (dec_features, layer_state, dec_hidden, dec_attn)
+        outputs = self.model(
+            input_ids=input_ids,
+            attention_mask=attention_mask,
+            position_ids=position_ids,
+            past_key_values=past_key_values,
+            inputs_embeds=inputs_embeds,
+            use_cache=use_cache,
+            output_attentions=output_attentions,
+            output_hidden_states=output_hidden_states,
+            return_dict=return_dict,
+            cache_position=cache_position,
+            **kwargs,
+        )
+
+        hidden_states = outputs[0]
+        # Only compute necessary logits,
+        # and do not upcast them to float if we are not computing the loss
+        logits = self.lm_head(hidden_states[:, -num_logits_to_keep:, :])
+
+        loss = None
+        if labels is not None:
+            loss = self.loss_function(
+                logits=logits, labels=labels,
+                vocab_size=self.config.vocab_size, **kwargs)
+
+        if not return_dict:
+            output = (logits,) + outputs[1:]
+            return (loss,) + output if loss is not None else output
+
+        return CausalLMOutputWithPast(
+            loss=loss,
+            logits=logits,
+            past_key_values=outputs.past_key_values,
+            hidden_states=outputs.hidden_states,
+            attentions=outputs.attentions,
+        )

Trained_20G/wkv.py

@@ -0,0 +1,603 @@
+import torch
+from einops import rearrange
+
+import math
+import torch.nn as nn
+from torch.nn import functional as F
+from .configuration_rwkv_hybrid import RwkvHybridConfig
+from typing import Optional
+from .hybrid_cache import HybridCache, AttnState, BlockState
+
+try:
+    import triton  # pylint: disable=F401
+    from rwkvfla.ops.rwkv7 import (
+        fused_recurrent_rwkv7,
+        chunk_rwkv7,
+        native_recurrent_rwkv7,
+        fused_addcmul_rwkv7,
+    )  # pylint: disable=C0411
+    from rwkvfla.ops.rwkv6 import (
+        fused_recurrent_rwkv6,
+        chunk_rwkv6,
+        native_recurrent_rwkv6,
+    )
+except ImportError:
+    from rwkvfla.ops.rwkv7 import native_recurrent_rwkv7  # pylint: disable=C0411
+    from rwkvfla.ops.rwkv6 import native_recurrent_rwkv6
+    from rwkvfla.ops.rwkv7 import torch_addcmul_rwkv7
+
+    fused_recurrent_rwkv7 = native_recurrent_rwkv7
+    chunk_rwkv7 = native_recurrent_rwkv7
+    chunk_rwkv6 = native_recurrent_rwkv6
+    fused_recurrent_rwkv6 = native_recurrent_rwkv6
+    fused_addcmul_rwkv7 = torch_addcmul_rwkv7
+
+from rwkvfla.utils import check_pytorch_version
+
+if check_pytorch_version("2.6"):
+    compile_decorator = torch.compile
+    torch._dynamo.config.cache_size_limit = 512
+else:
+    def compile_decorator(func):
+        return func
+
+
+class Rwkv_Tmix_x070(nn.Module):
+    def __init__(self, args: RwkvHybridConfig, layer_id, **kwargs):
+        super().__init__()
+        self.args = args
+        self.layer_id = layer_id
+        self.hidden_size = args.hidden_size
+
+        self.head_size = args.head_size
+        self.n_head = args.num_wkv_heads
+        assert args.hidden_size % self.n_head == 0
+        H = self.n_head
+        N = self.head_size
+
+        self.x_r = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.x_w = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.x_k = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.x_v = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.x_a = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+
+        D_DECAY_LORA = 64
+        D_AAA_LORA = 64
+        D_MV_LORA = 32
+        D_GATE_LORA = 128
+
+        self.w1 = nn.Parameter(torch.Tensor(args.hidden_size, D_DECAY_LORA))
+        self.w2 = nn.Parameter(torch.Tensor(D_DECAY_LORA, args.hidden_size))
+        self.w0 = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+
+        self.a1 = nn.Parameter(torch.Tensor(args.hidden_size, D_AAA_LORA))
+        self.a2 = nn.Parameter(torch.Tensor(D_AAA_LORA, args.hidden_size))
+        self.a0 = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+
+        self.v1 = nn.Parameter(torch.Tensor(args.hidden_size, D_MV_LORA))
+        self.v2 = nn.Parameter(torch.Tensor(D_MV_LORA, args.hidden_size))
+        self.v0 = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+
+        if self.args.wkv_has_gate:
+            self.x_g = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+            self.g1 = nn.Parameter(torch.Tensor(args.hidden_size, D_GATE_LORA))
+            self.g2 = nn.Parameter(torch.Tensor(D_GATE_LORA, args.hidden_size))
+
+        self.k_k = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.k_a = nn.Parameter(torch.Tensor(1, 1, args.hidden_size))
+        self.r_k = nn.Parameter(torch.Tensor(H, N))
+
+        self.time_shift = nn.ZeroPad2d((0, 0, 1, -1))
+        self.receptance = nn.Linear(
+            args.hidden_size, args.hidden_size, bias=False)
+        self.key = nn.Linear(args.hidden_size, args.hidden_size, bias=False)
+        self.value = nn.Linear(args.hidden_size, args.hidden_size, bias=False)
+        self.output = nn.Linear(args.hidden_size, args.hidden_size, bias=False)
+
+        if self.args.wkv_has_group_norm:
+            self.ln_x = nn.GroupNorm(
+                H, args.hidden_size, eps=(1e-5) * (args.head_size_divisor**2)
+            )
+
+    def post_init(self):
+        with torch.no_grad():
+            ratio_0_to_1 = self.layer_id / \
+                (self.args.num_hidden_layers - 1)  # 0 to 1
+            ratio_1_to_almost0 = 1.0 - (
+                self.layer_id / self.args.num_hidden_layers
+            )  # 1 to ~0
+
+            ddd = torch.ones(1, 1, self.args.hidden_size)
+            for i in range(self.args.hidden_size):
+                ddd[0, 0, i] = i / self.args.hidden_size
+
+            nn.init.constant_(
+                self.x_r, 1.0 - torch.pow(ddd, 0.2 * ratio_1_to_almost0))
+            nn.init.constant_(
+                self.x_w, 1.0 - torch.pow(ddd, 0.9 * ratio_1_to_almost0))
+            nn.init.constant_(
+                self.x_k,
+                1.0 - (torch.pow(ddd, 0.9 * ratio_1_to_almost0) +
+                       0.4 * ratio_0_to_1),
+            )
+            nn.init.constant_(
+                self.x_v,
+                1.0 - (torch.pow(ddd, 0.4 * ratio_1_to_almost0) +
+                       0.6 * ratio_0_to_1),
+            )
+            nn.init.constant_(
+                self.x_a, 1.0 - torch.pow(ddd, 0.9 * ratio_1_to_almost0))
+
+            def ortho_init(x, scale):
+                shape = x.shape
+                original_dtype = x.dtype
+                x_fp32 = x.float()
+                if len(shape) == 2:
+                    gain = math.sqrt(shape[0] / shape[1]
+                                     ) if shape[0] > shape[1] else 1
+                    nn.init.orthogonal_(x_fp32, gain=gain * scale)
+                elif len(shape) == 3:
+                    gain = math.sqrt(shape[1] / shape[2]
+                                     ) if shape[1] > shape[2] else 1
+                    for i in range(shape[0]):
+                        nn.init.orthogonal_(x_fp32[i], gain=gain * scale)
+                else:
+                    raise ValueError(
+                        "ortho_init only supports 2D or 3D tensors")
+                x.data.copy_(x_fp32.to(original_dtype))
+                return x
+
+            D_DECAY_LORA = 64
+            nn.init.zeros_(self.w1)
+            self.w2 = nn.Parameter(
+                ortho_init(torch.zeros(
+                    D_DECAY_LORA, self.args.hidden_size), 0.1)
+            )
+
+            decay_speed = torch.ones(self.args.hidden_size)
+            for n in range(self.args.hidden_size):
+                decay_speed[n] = -7 + 5 * (n / (self.args.hidden_size - 1)) ** (
+                    0.85 + 1.0 * ratio_0_to_1**0.5
+                )
+            nn.init.constant_(
+                self.w0, decay_speed.reshape(1, 1, self.args.hidden_size) + 0.5
+            )
+
+            D_AAA_LORA = 64
+            nn.init.zeros_(self.a1)
+            self.a2 = nn.Parameter(
+                ortho_init(torch.zeros(D_AAA_LORA, self.args.hidden_size), 0.1)
+            )
+            nn.init.zeros_(self.a0)
+
+            D_MV_LORA = 32
+            nn.init.zeros_(self.v1)
+            self.v2 = nn.Parameter(
+                ortho_init(torch.zeros(D_MV_LORA, self.args.hidden_size), 0.1)
+            )
+            nn.init.constant_(self.v0, 1.0)
+
+            D_GATE_LORA = 128
+            if self.args.wkv_has_gate:
+                nn.init.zeros_(self.g1)
+                self.g2 = nn.Parameter(
+                    ortho_init(torch.zeros(
+                        D_GATE_LORA, self.args.hidden_size), 0.1)
+                )
+                nn.init.constant_(
+                    self.x_g, 1.0 - torch.pow(ddd, 0.2 * ratio_1_to_almost0))
+
+            nn.init.constant_(self.k_k, 0.85)
+            nn.init.constant_(self.k_a, 1.0)
+            nn.init.zeros_(self.r_k)
+
+            nn.init.zeros_(self.receptance.weight)
+            nn.init.zeros_(self.key.weight)
+            nn.init.zeros_(self.value.weight)
+            nn.init.zeros_(self.output.weight)
+
+            if self.args.wkv_has_group_norm:
+                nn.init.ones_(self.ln_x.weight)
+                nn.init.zeros_(self.ln_x.bias)
+
+    def apply_wkv7_state(
+        self, r, k, v, w, a, b, s,
+        output_final_state,
+        cu_seqlens
+    ):
+        if r.device.type == "cpu":
+            r, w, k, v, a, b = map(lambda x: rearrange(
+                x, 'b l (h d) -> b h l d', h=self.n_head), (r, w, k, v, a, b))
+            o, state = native_recurrent_rwkv7(
+                r=r, k=k, v=v, w=w,
+                a=a, b=b,
+                scale=1.0,
+                initial_state=s.transpose(-1, -2),
+                output_final_state=True,
+                head_first=True,
+            )
+            state = state.transpose(-1, -2)
+            x = rearrange(o, "b h l d -> b l (h d)")
+        else:
+            r, w, k, v, a, b = map(lambda x: rearrange(
+                x, 'b l (h d) -> b l h d', h=self.n_head), (r, w, k, v, a, b))
+            wkv7_func = chunk_rwkv7 if r.shape[1] != 1 else fused_recurrent_rwkv7
+            o, state = wkv7_func(
+                r=r, k=k, v=v, w=w,
+                a=a, b=b,
+                scale=1.0,
+                initial_state=s,
+                output_final_state=output_final_state,
+                cu_seqlens=cu_seqlens,
+                head_first=False,
+            )
+            x = rearrange(o, "b l h d -> b l (h d)")
+        return x, state
+
+    @compile_decorator
+    def forward(
+            self,
+            hidden_states,
+            last_state: AttnState,
+            use_cache: Optional[bool] = False,
+            cu_seqlens: Optional[torch.Tensor] = None,
+            v_first: Optional[torch.Tensor] = None,
+            attention_mask: Optional[torch.Tensor] = None,
+            **kwargs
+    ):
+        shift_state = last_state.shift_state
+        B, T, C = hidden_states.size()
+
+        xx = torch.concat((shift_state.unsqueeze(
+            1), hidden_states[:, :-1]), dim=1) - hidden_states
+
+        lx = hidden_states[:, -1]
+
+        if self.args.wkv_has_gate:
+            xr, xw, xk, xv, xa, xg = fused_addcmul_rwkv7(
+                hidden_states, xx, self.x_r, self.x_w, self.x_k, self.x_v, self.x_a, self.x_g)
+        else:
+            xr, xw, xk, xv, xa, _ = fused_addcmul_rwkv7(
+                hidden_states, xx, self.x_r, self.x_w, self.x_k, self.x_v, self.x_a)
+
+        r = self.receptance(xr)
+        w = (
+            -F.softplus(-(self.w0 + torch.tanh(xw @ self.w1) @ self.w2)) - 0.5
+        )  # soft-clamp to (-inf, -0.5)
+        k = self.key(xk)
+        v = self.value(xv)
+        if self.layer_id == 0:
+            v_first = v
+        else:
+            v = torch.lerp(v, v_first, torch.sigmoid(
+                self.v0 + (xv @ self.v1) @ self.v2
+            ))  # add value residual
+
+        if attention_mask is not None:
+            v = v.mul(attention_mask[:, -v.shape[-2]:, None])
+        a = torch.sigmoid(
+            self.a0 + (xa @ self.a1) @ self.a2
+        )  # a is "in-context learning rate"
+        if self.args.wkv_has_gate:
+            g = torch.sigmoid(xg @ self.g1) @ self.g2 + 1.0
+        kk = k * self.k_k
+        kk = F.normalize(kk.view(B, T, self.n_head, -1),
+                         p=2.0, dim=-1, eps=1e-4 if kk.dtype == torch.float16 else 1e-12).view(B, T, C)
+        k = torch.lerp(k, k * a, self.k_a)
+
+        wkv_state = last_state.wkv_state
+        hidden_states, wkv_state = self.apply_wkv7_state(
+            r,
+            k,
+            v,
+            w,
+            -kk,
+            (kk * a),
+            s=wkv_state,
+            output_final_state=use_cache,
+            cu_seqlens=cu_seqlens
+        )
+        if self.args.wkv_has_group_norm:
+            hidden_states = self.ln_x(
+                hidden_states.view(B * T, C)).view(B, T, C)
+
+        # original code:
+        # weighted_sum_rk = (r.view(B, T, self.n_head, -1) * k.view(B, T, self.n_head, -1) * self.r_k).sum(
+        #         dim=-1, keepdim=True
+        #     )
+        weighted_sum_rk = torch.einsum('btij,btij,ij->btij', r.view(B, T, self.n_head, -1),
+                                       k.view(B, T, self.n_head, -1), self.r_k).sum(dim=-1, keepdim=True)
+        hidden_states = hidden_states + \
+            (weighted_sum_rk * v.view(B, T, self.n_head, -1)).view(B, T, C)
+        hidden_states = self.output(
+            hidden_states * g) if self.args.wkv_has_gate else self.output(hidden_states)
+        return hidden_states, AttnState(lx, wkv_state), v_first
+
+
+class Rwkv7Attention(nn.Module):
+    def __init__(self, args: RwkvHybridConfig, layer_id):
+        super().__init__()
+        self.args = args
+        self.layer_idx = layer_id
+        self.time_mixer = Rwkv_Tmix_x070(args, layer_id)
+
+    def forward(
+        self,
+        hidden_states: torch.Tensor,
+        attention_mask: Optional[torch.Tensor] = None,
+        position_ids: Optional[torch.Tensor] = None,
+        past_key_value: Optional[HybridCache] = None,
+        output_attentions: Optional[bool] = False,
+        use_cache: Optional[bool] = False,
+        cache_position: Optional[torch.Tensor] = None,
+        position_embeddings: Optional[torch.Tensor] = None,
+        cu_seqlens: Optional[torch.Tensor] = None,
+        v_first: Optional[torch.Tensor] = None,
+        **kwargs
+    ):
+
+        batch_size, token_length, _ = hidden_states.shape
+
+        if use_cache and len(past_key_value) > self.layer_idx:
+            last_state = past_key_value[self.layer_idx][0]
+        else:
+            last_state = self.init_state(
+                batch_size, hidden_states.device, hidden_states.dtype
+            )
+
+        attn_output, states, v_first = self.time_mixer(hidden_states=hidden_states,
+                                                       last_state=last_state.attn_state,
+                                                       use_cache=use_cache,
+                                                       cu_seqlens=cu_seqlens,
+                                                       v_first=v_first,
+                                                       **kwargs)
+
+        if use_cache:
+            last_state.attn_state = states
+            past_key_value.update(token_length, last_state, self.layer_idx)
+
+        return attn_output, None, v_first
+
+    def init_state(self, batch_size, device, dtype) -> BlockState:
+        wkv_states = torch.zeros(
+            (
+                batch_size,
+                self.args.num_wkv_heads,
+                self.args.head_size,
+                self.args.head_size,
+            ),
+            device=device,
+            dtype=torch.float32,
+        )
+        shift_states = torch.zeros(
+            (batch_size, self.args.hidden_size), device=device, dtype=dtype
+        )
+        return BlockState(AttnState(shift_states, wkv_states), None)
+
+
+class Rwkv_Tmix_x060(nn.Module):
+    def __init__(self, args: RwkvHybridConfig, layer_id, **kwargs):
+        super().__init__()
+        self.args = args
+        self.layer_id = layer_id
+        self.hidden_size = args.hidden_size
+
+        self.head_size = args.head_size
+        self.n_head = args.num_wkv_heads
+        assert args.hidden_size % self.n_head == 0
+
+        with torch.no_grad():
+            ratio_0_to_1 = layer_id / (args.n_layer - 1)  # 0 to 1
+            ratio_1_to_almost0 = 1.0 - (layer_id / args.n_layer)  # 1 to ~0
+            ddd = torch.ones(1, 1, args.hidden_size)
+            for i in range(args.hidden_size):
+                ddd[0, 0, i] = i / args.hidden_size
+
+            # fancy time_mix
+            self.time_maa_x = nn.Parameter(
+                1.0 - torch.pow(ddd, ratio_1_to_almost0))
+            self.time_maa_w = nn.Parameter(
+                1.0 - torch.pow(ddd, ratio_1_to_almost0))
+            self.time_maa_k = nn.Parameter(
+                1.0 - torch.pow(ddd, ratio_1_to_almost0))
+            self.time_maa_v = nn.Parameter(
+                1.0 - (torch.pow(ddd, ratio_1_to_almost0) + 0.3 * ratio_0_to_1)
+            )
+            self.time_maa_r = nn.Parameter(
+                1.0 - torch.pow(ddd, 0.5 * ratio_1_to_almost0)
+            )
+            self.time_maa_g = nn.Parameter(
+                1.0 - torch.pow(ddd, 0.5 * ratio_1_to_almost0)
+            )
+
+            D_MIX_LORA = 32  # generate TIME_MIX for w,k,v,r,g
+            if args.hidden_size == 4096:
+                D_MIX_LORA = D_MIX_LORA * 2
+            self.time_maa_w1 = nn.Parameter(
+                torch.zeros(args.hidden_size, D_MIX_LORA * 5)
+            )
+            self.time_maa_w2 = nn.Parameter(
+                torch.zeros(5, D_MIX_LORA,
+                            args.hidden_size).uniform_(-0.01, 0.01)
+            )
+
+            # fancy time_decay
+            decay_speed = torch.ones(args.head_size)
+            for n in range(args.head_size):
+                decay_speed[n] = -6 + 5 * (n / (args.head_size - 1)) ** (
+                    0.7 + 1.3 * ratio_0_to_1
+                )
+            self.time_decay = nn.Parameter(
+                decay_speed.reshape(1, 1, args.head_size))
+
+            D_DECAY_LORA = 64
+            if args.hidden_size == 4096:
+                D_DECAY_LORA = D_DECAY_LORA * 2
+            self.time_decay_w1 = nn.Parameter(
+                torch.zeros(args.hidden_size, D_DECAY_LORA)
+            )
+            self.time_decay_w2 = nn.Parameter(
+                torch.zeros(D_DECAY_LORA, args.head_size).uniform_(-0.01, 0.01)
+            )
+
+            tmp = torch.zeros(args.head_size)
+            for n in range(args.head_size):
+                zigzag = ((n + 1) % 3 - 1) * 0.1
+                tmp[n] = ratio_0_to_1 * \
+                    (1 - (n / (args.head_size - 1))) + zigzag
+
+            self.time_faaaa = nn.Parameter(
+                tmp.reshape(self.n_head, self.head_size))
+
+        self.time_shift = nn.ZeroPad2d((0, 0, 1, -1))
+        self.receptance = nn.Linear(
+            args.hidden_size, args.head_size, bias=False)
+        self.key = nn.Linear(args.hidden_size, args.head_size, bias=False)
+
+        self.value = nn.Linear(args.hidden_size, args.head_size, bias=False)
+        self.output = nn.Linear(args.head_size, args.hidden_size, bias=False)
+        self.gate = nn.Linear(args.hidden_size, args.head_size, bias=False)
+
+        if self.args.wkv_has_group_norm:
+            self.ln_x = nn.GroupNorm(
+                self.n_head, args.head_size, eps=(
+                    1e-5) * (args.head_size_divisor**2)
+            )
+
+    def post_init(self):
+        pass
+
+    @compile_decorator
+    def forward(
+        self,
+        hidden_states,
+        last_state: AttnState,
+        use_cache: Optional[bool] = False,
+        cu_seqlens: Optional[torch.Tensor] = None,
+        v_first: Optional[torch.Tensor] = None,
+        **kwargs
+    ):
+        shift_state = last_state.shift_state
+        B, T, C = hidden_states.size()
+        H = self.n_head
+
+        xx = torch.concat((shift_state.unsqueeze(
+            1), hidden_states[:, :-1]), dim=1) - hidden_states
+
+        lx = hidden_states[:, -1]
+
+        xxx = hidden_states + xx * self.time_maa_x
+        xxx = torch.tanh(xxx @ self.time_maa_w1).view(B *
+                                                      T, 5, -1).transpose(0, 1)
+        xxx = torch.bmm(xxx, self.time_maa_w2).view(5, B, T, -1)
+        mw, mk, mv, mr, mg = xxx.unbind(dim=0)
+
+        xw = hidden_states + xx * (self.time_maa_w + mw)
+        xk = hidden_states + xx * (self.time_maa_k + mk)
+        xv = hidden_states + xx * (self.time_maa_v + mv)
+        xr = hidden_states + xx * (self.time_maa_r + mr)
+        xg = hidden_states + xx * (self.time_maa_g + mg)
+
+        r = self.receptance(xr)
+        k = self.key(xk)
+        v = self.value(xv)
+        g = F.silu(self.gate(xg))
+
+        ww = torch.tanh(xw @ self.time_decay_w1) @ self.time_decay_w2
+        w = self.time_decay + ww
+
+        wkv_state = last_state.wkv_state
+        hidden_states, wkv_state = self.apply_wkv6_state(
+            B, T, C, H, r, k, v, w, u=self.time_faaaa, s=wkv_state
+        )
+        if self.args.wkv_has_group_norm:
+            hidden_states = self.ln_x(
+                hidden_states.view(B * T, C)).view(B, T, C)
+        hidden_states = self.output(hidden_states * g)
+        return hidden_states, AttnState(lx, wkv_state), None
+
+    def apply_wkv6_state(self, B, T, C, H, r, k, v, w, u, s):
+        r, w, k, v = map(lambda x: rearrange(
+            x, 'b l (h d) -> b h l d', h=self.n_head), (r, w, k, v))
+
+        if r.device.type == "cpu":
+            wkv6_func = native_recurrent_rwkv6
+        elif self.training:
+            wkv6_func = chunk_rwkv6
+        else:
+            wkv6_func = fused_recurrent_rwkv6
+
+        o, state = wkv6_func(
+            r,
+            k,
+            v,
+            -torch.exp(w),
+            u=u,
+            scale=1.0,
+            initial_state=s,
+            output_final_state=True,
+        )
+        x = rearrange(o, "b h l d -> b l (h d)")
+        return x, state
+
+
+class Rwkv6Attention(nn.Module):
+    def __init__(self, args: RwkvHybridConfig, layer_id, **kwargs):
+        super().__init__()
+        self.args = args
+        self.layer_idx = layer_id
+        self.time_mixer = Rwkv_Tmix_x060(args, layer_id, **kwargs)
+
+    def forward(
+        self,
+        hidden_states: torch.Tensor,
+        attention_mask: Optional[torch.Tensor] = None,
+        position_ids: Optional[torch.Tensor] = None,
+        past_key_value: Optional[HybridCache] = None,
+        output_attentions: Optional[bool] = False,
+        use_cache: Optional[bool] = False,
+        cache_position: Optional[torch.Tensor] = None,
+        position_embeddings: Optional[torch.Tensor] = None,
+        cu_seqlens: Optional[torch.Tensor] = None,
+        v_first: Optional[torch.Tensor] = None,
+        **kwargs
+    ):
+        attn_output = hidden_states
+
+        batch_size, token_length, _ = hidden_states.shape
+
+        if use_cache and len(past_key_value) > self.layer_idx:
+            last_state = past_key_value[self.layer_idx][0]
+        else:
+            last_state = self.init_state(
+                batch_size, hidden_states.device, hidden_states.dtype
+            )
+        
+        attn_output, states, v_first = self.time_mixer(hidden_states=hidden_states,
+                                                       last_state=last_state.attn_state,
+                                                       use_cache=use_cache,
+                                                       cu_seqlens=cu_seqlens,
+                                                       v_first=v_first,
+                                                       **kwargs)
+
+        if use_cache:
+            last_state.attn_state = states
+            past_key_value.update(token_length, last_state, self.layer_idx)
+
+        return attn_output, None, v_first
+    
+    def init_state(self, batch_size, device, dtype) -> BlockState:
+        wkv_states = torch.zeros(
+            (
+                batch_size,
+                self.args.num_wkv_heads,
+                self.args.head_size,
+                self.args.head_size,
+            ),
+            device=device,
+            dtype=torch.float32,
+        )
+        shift_states = torch.zeros(
+            (batch_size, self.args.hidden_size), device=device, dtype=dtype
+        )
+        return BlockState(AttnState(shift_states, wkv_states), None)